MLIR

Multi-Level IR Compiler Framework

'rocdl' Dialect

Operation definition 

rocdl.barrier (::mlir::ROCDL::BarrierOp) 

Syntax:

operation ::= `rocdl.barrier` attr-dict

rocdl.workgroup.dim.x (::mlir::ROCDL::BlockDimXOp) 

Syntax:

operation ::= `rocdl.workgroup.dim.x` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.workgroup.dim.y (::mlir::ROCDL::BlockDimYOp) 

Syntax:

operation ::= `rocdl.workgroup.dim.y` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.workgroup.dim.z (::mlir::ROCDL::BlockDimZOp) 

Syntax:

operation ::= `rocdl.workgroup.dim.z` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.workgroup.id.x (::mlir::ROCDL::BlockIdXOp) 

Syntax:

operation ::= `rocdl.workgroup.id.x` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.workgroup.id.y (::mlir::ROCDL::BlockIdYOp) 

Syntax:

operation ::= `rocdl.workgroup.id.y` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.workgroup.id.z (::mlir::ROCDL::BlockIdZOp) 

Syntax:

operation ::= `rocdl.workgroup.id.z` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.grid.dim.x (::mlir::ROCDL::GridDimXOp) 

Syntax:

operation ::= `rocdl.grid.dim.x` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.grid.dim.y (::mlir::ROCDL::GridDimYOp) 

Syntax:

operation ::= `rocdl.grid.dim.y` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.grid.dim.z (::mlir::ROCDL::GridDimZOp) 

Syntax:

operation ::= `rocdl.grid.dim.z` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.buffer.load (::mlir::ROCDL::MubufLoadOp) 

Operands: 

OperandDescription
rsrcLLVM dialect type
vindexLLVM dialect type
offsetLLVM dialect type
glcLLVM dialect type
slcLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.buffer.store (::mlir::ROCDL::MubufStoreOp) 

Operands: 

OperandDescription
vdataLLVM dialect type
rsrcLLVM dialect type
vindexLLVM dialect type
offsetLLVM dialect type
glcLLVM dialect type
slcLLVM dialect type

rocdl.workitem.id.x (::mlir::ROCDL::ThreadIdXOp) 

Syntax:

operation ::= `rocdl.workitem.id.x` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.workitem.id.y (::mlir::ROCDL::ThreadIdYOp) 

Syntax:

operation ::= `rocdl.workitem.id.y` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.workitem.id.z (::mlir::ROCDL::ThreadIdZOp) 

Syntax:

operation ::= `rocdl.workitem.id.z` attr-dict `:` type($res)

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.16x16x16f16 (::mlir::ROCDL::mfma_f32_16x16x16f16) 

Syntax:

operation ::= `rocdl.mfma.f32.16x16x16f16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.16x16x1f32 (::mlir::ROCDL::mfma_f32_16x16x1f32) 

Syntax:

operation ::= `rocdl.mfma.f32.16x16x1f32` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.16x16x2bf16 (::mlir::ROCDL::mfma_f32_16x16x2bf16) 

Syntax:

operation ::= `rocdl.mfma.f32.16x16x2bf16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.16x16x4f16 (::mlir::ROCDL::mfma_f32_16x16x4f16) 

Syntax:

operation ::= `rocdl.mfma.f32.16x16x4f16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.16x16x4f32 (::mlir::ROCDL::mfma_f32_16x16x4f32) 

Syntax:

operation ::= `rocdl.mfma.f32.16x16x4f32` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.16x16x8bf16 (::mlir::ROCDL::mfma_f32_16x16x8bf16) 

Syntax:

operation ::= `rocdl.mfma.f32.16x16x8bf16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.32x32x1f32 (::mlir::ROCDL::mfma_f32_32x32x1f32) 

Syntax:

operation ::= `rocdl.mfma.f32.32x32x1f32` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.32x32x2bf16 (::mlir::ROCDL::mfma_f32_32x32x2bf16) 

Syntax:

operation ::= `rocdl.mfma.f32.32x32x2bf16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.32x32x2f32 (::mlir::ROCDL::mfma_f32_32x32x2f32) 

Syntax:

operation ::= `rocdl.mfma.f32.32x32x2f32` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.32x32x4bf16 (::mlir::ROCDL::mfma_f32_32x32x4bf16) 

Syntax:

operation ::= `rocdl.mfma.f32.32x32x4bf16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.32x32x4f16 (::mlir::ROCDL::mfma_f32_32x32x4f16) 

Syntax:

operation ::= `rocdl.mfma.f32.32x32x4f16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.32x32x8f16 (::mlir::ROCDL::mfma_f32_32x32x8f16) 

Syntax:

operation ::= `rocdl.mfma.f32.32x32x8f16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.4x4x1f32 (::mlir::ROCDL::mfma_f32_4x4x1f32) 

Syntax:

operation ::= `rocdl.mfma.f32.4x4x1f32` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.4x4x2bf16 (::mlir::ROCDL::mfma_f32_4x4x2bf16) 

Syntax:

operation ::= `rocdl.mfma.f32.4x4x2bf16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.f32.4x4x4f16 (::mlir::ROCDL::mfma_f32_4x4x4f16) 

Syntax:

operation ::= `rocdl.mfma.f32.4x4x4f16` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.i32.16x16x16i8 (::mlir::ROCDL::mfma_i32_16x16x16i8) 

Syntax:

operation ::= `rocdl.mfma.i32.16x16x16i8` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.i32.16x16x4i8 (::mlir::ROCDL::mfma_i32_16x16x4i8) 

Syntax:

operation ::= `rocdl.mfma.i32.16x16x4i8` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.i32.32x32x4i8 (::mlir::ROCDL::mfma_i32_32x32x4i8) 

Syntax:

operation ::= `rocdl.mfma.i32.32x32x4i8` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.i32.32x32x8i8 (::mlir::ROCDL::mfma_i32_32x32x8i8) 

Syntax:

operation ::= `rocdl.mfma.i32.32x32x8i8` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type

rocdl.mfma.i32.4x4x4i8 (::mlir::ROCDL::mfma_i32_4x4x4i8) 

Syntax:

operation ::= `rocdl.mfma.i32.4x4x4i8` $args attr-dict `:` functional-type($args, $res)

Operands: 

OperandDescription
argsLLVM dialect type

Results: 

ResultDescription
resLLVM dialect type