tilelang.cuda.op.gemm.gemm_mma_sm70¶

Attributes¶

GEMM_INST_MMA

Classes¶

GemmMMASm70

Base class for GEMM tile operators.

Module Contents¶

tilelang.cuda.op.gemm.gemm_mma_sm70.GEMM_INST_MMA = 'cuda.mma'¶
class tilelang.cuda.op.gemm.gemm_mma_sm70.GemmMMASm70¶

Bases: tilelang.tileop.gemm.gemm_base.GemmBase

Base class for GEMM tile operators.

Classifies the GEMM variant by the memory scopes of operands A and B (SS, SR, RS, TS, RR) and provides common property accessors for the underlying gemm_node IR node.

infer_layout(target, thread_nums)¶
Parameters:

  • target (tvm.target.Target)

  • thread_nums (int)

lower(layout_map, target, thread_bounds, thread_var, mbar_phase_expr=None)¶
Parameters:

  • layout_map (dict)

  • target (tvm.target.Target)

  • thread_bounds (tvm.ir.Range)

  • thread_var (tvm.tirx.Var)

  • mbar_phase_expr (tvm.tirx.PrimExpr | None)