TT-MLIR
|
Public Types | |
using | Adaptor = EnqueueProgramOpAdaptor |
template<typename RangeT > | |
using | GenericAdaptor = EnqueueProgramOpGenericAdaptor< RangeT > |
using | FoldAdaptor = GenericAdaptor<::llvm::ArrayRef<::mlir::Attribute > > |
using | Properties = FoldAdaptor::Properties |
Public Member Functions | |
static ::llvm::ArrayRef<::llvm::StringRef > | getAttributeNames () |
::mlir::StringAttr | getCbPortsAttrName () |
::mlir::StringAttr | getKernelConfigsAttrName () |
::mlir::StringAttr | getOperandSegmentSizesAttrName () |
std::pair< unsigned, unsigned > | getODSOperandIndexAndLength (unsigned index) |
::mlir::Operation::operand_range | getODSOperands (unsigned index) |
::mlir::Operation::operand_range | getBuffers () |
::mlir::Operation::operand_range | getCbs () |
::mlir::MutableOperandRange | getBuffersMutable () |
::mlir::MutableOperandRange | getCbsMutable () |
std::pair< unsigned, unsigned > | getODSResultIndexAndLength (unsigned index) |
::mlir::Operation::result_range | getODSResults (unsigned index) |
void | writeProperties (::mlir::DialectBytecodeWriter &writer) |
::mlir::DenseI64ArrayAttr | getCbPortsAttr () |
::llvm::ArrayRef< int64_t > | getCbPorts () |
::mlir::ArrayAttr | getKernelConfigsAttr () |
::mlir::ArrayAttr | getKernelConfigs () |
void | setCbPortsAttr (::mlir::DenseI64ArrayAttr attr) |
void | setCbPorts (::llvm::ArrayRef< int64_t > attrValue) |
void | setKernelConfigsAttr (::mlir::ArrayAttr attr) |
::llvm::LogicalResult | verifyInvariantsImpl () |
::llvm::LogicalResult | verifyInvariants () |
::llvm::LogicalResult | verify () |
void | getEffects (::llvm::SmallVectorImpl<::mlir::SideEffects::EffectInstance<::mlir::MemoryEffects::Effect >> &effects) |
Static Public Member Functions | |
::mlir::StringAttr | getCbPortsAttrName (::mlir::OperationName name) |
::mlir::StringAttr | getKernelConfigsAttrName (::mlir::OperationName name) |
::mlir::StringAttr | getOperandSegmentSizesAttrName (::mlir::OperationName name) |
static constexpr ::llvm::StringLiteral | getOperationName () |
::llvm::LogicalResult | setPropertiesFromAttr (Properties &prop, ::mlir::Attribute attr, ::llvm::function_ref<::mlir::InFlightDiagnostic()> emitError) |
::mlir::Attribute | getPropertiesAsAttr (::mlir::MLIRContext *ctx, const Properties &prop) |
static llvm::hash_code | computePropertiesHash (const Properties &prop) |
static std::optional< mlir::Attribute > | getInherentAttr (::mlir::MLIRContext *ctx, const Properties &prop, llvm::StringRef name) |
static void | setInherentAttr (Properties &prop, llvm::StringRef name, mlir::Attribute value) |
static void | populateInherentAttrs (::mlir::MLIRContext *ctx, const Properties &prop, ::mlir::NamedAttrList &attrs) |
::llvm::LogicalResult | verifyInherentAttrs (::mlir::OperationName opName, ::mlir::NamedAttrList &attrs, llvm::function_ref<::mlir::InFlightDiagnostic()> emitError) |
::llvm::LogicalResult | readProperties (::mlir::DialectBytecodeReader &reader, ::mlir::OperationState &state) |
static void | build (::mlir::OpBuilder &odsBuilder, ::mlir::OperationState &odsState, ::mlir::ValueRange buffers, ::mlir::ValueRange cbs, ::mlir::DenseI64ArrayAttr cb_ports, ::mlir::ArrayAttr kernelConfigs) |
static void | build (::mlir::OpBuilder &odsBuilder, ::mlir::OperationState &odsState, ::mlir::TypeRange resultTypes, ::mlir::ValueRange buffers, ::mlir::ValueRange cbs, ::mlir::DenseI64ArrayAttr cb_ports, ::mlir::ArrayAttr kernelConfigs) |
static void | build (::mlir::OpBuilder &odsBuilder, ::mlir::OperationState &odsState, ::mlir::ValueRange buffers, ::mlir::ValueRange cbs, ::llvm::ArrayRef< int64_t > cb_ports, ::mlir::ArrayAttr kernelConfigs) |
static void | build (::mlir::OpBuilder &odsBuilder, ::mlir::OperationState &odsState, ::mlir::TypeRange resultTypes, ::mlir::ValueRange buffers, ::mlir::ValueRange cbs, ::llvm::ArrayRef< int64_t > cb_ports, ::mlir::ArrayAttr kernelConfigs) |
static void | build (::mlir::OpBuilder &, ::mlir::OperationState &odsState, ::mlir::TypeRange resultTypes, ::mlir::ValueRange operands, ::llvm::ArrayRef<::mlir::NamedAttribute > attributes={}) |
Private Member Functions | |
::mlir::StringAttr | getAttributeNameForIndex (unsigned index) |
Static Private Member Functions | |
::mlir::StringAttr | getAttributeNameForIndex (::mlir::OperationName name, unsigned index) |
using mlir::tt::ttmetal::EnqueueProgramOp::FoldAdaptor = GenericAdaptor<::llvm::ArrayRef<::mlir::Attribute> > |
using mlir::tt::ttmetal::EnqueueProgramOp::GenericAdaptor = EnqueueProgramOpGenericAdaptor<RangeT> |
|
static |
|
static |
|
static |
|
static |
|
static |
|
static |
|
inlinestaticprivate |
|
inlineprivate |
|
inline |
|
inline |
mlir::MutableOperandRange mlir::tt::ttmetal::EnqueueProgramOp::getBuffersMutable | ( | ) |
llvm::ArrayRef< int64_t > mlir::tt::ttmetal::EnqueueProgramOp::getCbPorts | ( | ) |
|
inline |
|
inline |
|
inlinestatic |
|
inline |
mlir::MutableOperandRange mlir::tt::ttmetal::EnqueueProgramOp::getCbsMutable | ( | ) |
void mlir::tt::ttmetal::EnqueueProgramOp::getEffects | ( | ::llvm::SmallVectorImpl<::mlir::SideEffects::EffectInstance<::mlir::MemoryEffects::Effect >> & | effects | ) |
|
static |
mlir::ArrayAttr mlir::tt::ttmetal::EnqueueProgramOp::getKernelConfigs | ( | ) |
|
inline |
|
inline |
|
inlinestatic |
std::pair< unsigned, unsigned > mlir::tt::ttmetal::EnqueueProgramOp::getODSOperandIndexAndLength | ( | unsigned | index | ) |
|
inline |
|
inline |
|
inline |
|
inline |
|
inlinestatic |
|
inlinestatic |
|
static |
|
static |
|
static |
void mlir::tt::ttmetal::EnqueueProgramOp::setCbPorts | ( | ::llvm::ArrayRef< int64_t > | attrValue | ) |
|
inline |
|
static |
|
inline |
|
static |
::llvm::LogicalResult mlir::tt::ttmetal::EnqueueProgramOp::verify | ( | ) |
|
static |
llvm::LogicalResult mlir::tt::ttmetal::EnqueueProgramOp::verifyInvariants | ( | ) |
llvm::LogicalResult mlir::tt::ttmetal::EnqueueProgramOp::verifyInvariantsImpl | ( | ) |
void mlir::tt::ttmetal::EnqueueProgramOp::writeProperties | ( | ::mlir::DialectBytecodeWriter & | writer | ) |