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