'nvvm' Dialect
Operation definition
nvvm.barrier0 (NVVM::Barrier0Op)
Syntax:
operation ::= `nvvm.barrier0` attr-dict
nvvm.read.ptx.sreg.ntid.x (NVVM::BlockDimXOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.ntid.x` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.ntid.y (NVVM::BlockDimYOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.ntid.y` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.ntid.z (NVVM::BlockDimZOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.ntid.z` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.ctaid.x (NVVM::BlockIdXOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.ctaid.x` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.ctaid.y (NVVM::BlockIdYOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.ctaid.y` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.ctaid.z (NVVM::BlockIdZOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.ctaid.z` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.nctaid.x (NVVM::GridDimXOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.nctaid.x` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.nctaid.y (NVVM::GridDimYOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.nctaid.y` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.nctaid.z (NVVM::GridDimZOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.nctaid.z` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.laneid (NVVM::LaneIdOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.laneid` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.mma.sync (NVVM::MmaOp)
Syntax:
operation ::= `nvvm.mma.sync` $args attr-dict `:` functional-type($args, $res)
Operands:
| Operand | Description |
|---|
args | LLVM dialect type |
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.shfl.sync.bfly (NVVM::ShflBflyOp)
Attributes:
| Attribute | MLIR Type | Description |
|---|
return_value_and_is_valid | UnitAttr | unit attribute |
Operands:
| Operand | Description |
|---|
dst | LLVM dialect type |
val | LLVM dialect type |
offset | LLVM dialect type |
mask_and_clamp | LLVM dialect type |
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.tid.x (NVVM::ThreadIdXOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.tid.x` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.tid.y (NVVM::ThreadIdYOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.tid.y` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.tid.z (NVVM::ThreadIdZOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.tid.z` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.vote.ballot.sync (NVVM::VoteBallotOp)
Operands:
| Operand | Description |
|---|
mask | LLVM dialect type |
pred | LLVM dialect type |
Results:
| Result | Description |
|---|
res | LLVM dialect type |
nvvm.read.ptx.sreg.warpsize (NVVM::WarpSizeOp)
Syntax:
operation ::= `nvvm.read.ptx.sreg.warpsize` attr-dict `:` type($res)
Results:
| Result | Description |
|---|
res | LLVM dialect type |
MLIR