MLIR

Multi-Level IR Compiler Framework

'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:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.ntid.y (NVVM::BlockDimYOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.ntid.y` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.ntid.z (NVVM::BlockDimZOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.ntid.z` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.ctaid.x (NVVM::BlockIdXOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.ctaid.x` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.ctaid.y (NVVM::BlockIdYOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.ctaid.y` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.ctaid.z (NVVM::BlockIdZOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.ctaid.z` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.nctaid.x (NVVM::GridDimXOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.nctaid.x` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.nctaid.y (NVVM::GridDimYOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.nctaid.y` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.nctaid.z (NVVM::GridDimZOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.nctaid.z` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.laneid (NVVM::LaneIdOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.laneid` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.mma.sync (NVVM::MmaOp)

Syntax:

operation ::= `nvvm.mma.sync` $args attr-dict `:` functional-type($args, $res)

Operands:

OperandDescription
argsLLVM dialect type

Results:

ResultDescription
resLLVM dialect type

nvvm.shfl.sync.bfly (NVVM::ShflBflyOp)

Attributes:

AttributeMLIR TypeDescription
return_value_and_is_validUnitAttrunit attribute

Operands:

OperandDescription
dstLLVM dialect type
valLLVM dialect type
offsetLLVM dialect type
mask_and_clampLLVM dialect type

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.tid.x (NVVM::ThreadIdXOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.tid.x` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.tid.y (NVVM::ThreadIdYOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.tid.y` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.tid.z (NVVM::ThreadIdZOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.tid.z` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type

nvvm.vote.ballot.sync (NVVM::VoteBallotOp)

Operands:

OperandDescription
maskLLVM dialect type
predLLVM dialect type

Results:

ResultDescription
resLLVM dialect type

nvvm.read.ptx.sreg.warpsize (NVVM::WarpSizeOp)

Syntax:

operation ::= `nvvm.read.ptx.sreg.warpsize` attr-dict `:` type($res)

Results:

ResultDescription
resLLVM dialect type