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 | getCoreRangesAttrName () |
::mlir::StringAttr | getKernelConfigsAttrName () |
::mlir::StringAttr | getThreadsAttrName () |
::mlir::StringAttr | getOperandSegmentSizesAttrName () |
std::pair< unsigned, unsigned > | getODSOperandIndexAndLength (unsigned index) |
::mlir::Operation::operand_range | getODSOperands (unsigned index) |
::mlir::Operation::operand_range | getInputs () |
::mlir::Operation::operand_range | getOutputs () |
::mlir::MutableOperandRange | getInputsMutable () |
::mlir::MutableOperandRange | getOutputsMutable () |
std::pair< unsigned, unsigned > | getODSResultIndexAndLength (unsigned index) |
::mlir::Operation::result_range | getODSResults (unsigned index) |
void | writeProperties (::mlir::DialectBytecodeWriter &writer) |
::mlir::ArrayAttr | getThreadsAttr () |
::mlir::ArrayAttr | getThreads () |
::mlir::ArrayAttr | getCoreRangesAttr () |
::mlir::ArrayAttr | getCoreRanges () |
::mlir::ArrayAttr | getKernelConfigsAttr () |
::mlir::ArrayAttr | getKernelConfigs () |
void | setThreadsAttr (::mlir::ArrayAttr attr) |
void | setCoreRangesAttr (::mlir::ArrayAttr attr) |
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 | getCoreRangesAttrName (::mlir::OperationName name) |
::mlir::StringAttr | getKernelConfigsAttrName (::mlir::OperationName name) |
::mlir::StringAttr | getThreadsAttrName (::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 inputs, ::mlir::ValueRange outputs, ::mlir::ArrayAttr threads, ::mlir::ArrayAttr core_ranges, ::mlir::ArrayAttr kernelConfigs) |
static void | build (::mlir::OpBuilder &odsBuilder, ::mlir::OperationState &odsState, ::mlir::TypeRange resultTypes, ::mlir::ValueRange inputs, ::mlir::ValueRange outputs, ::mlir::ArrayAttr threads, ::mlir::ArrayAttr core_ranges, ::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 |
|
inlinestaticprivate |
|
inlineprivate |
|
inline |
mlir::ArrayAttr mlir::tt::ttmetal::EnqueueProgramOp::getCoreRanges | ( | ) |
|
inline |
|
inline |
|
inlinestatic |
void mlir::tt::ttmetal::EnqueueProgramOp::getEffects | ( | ::llvm::SmallVectorImpl<::mlir::SideEffects::EffectInstance<::mlir::MemoryEffects::Effect >> & | effects | ) |
|
static |
|
inline |
mlir::MutableOperandRange mlir::tt::ttmetal::EnqueueProgramOp::getInputsMutable | ( | ) |
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 |
|
inline |
mlir::MutableOperandRange mlir::tt::ttmetal::EnqueueProgramOp::getOutputsMutable | ( | ) |
|
static |
mlir::ArrayAttr mlir::tt::ttmetal::EnqueueProgramOp::getThreads | ( | ) |
|
inline |
|
inline |
|
inlinestatic |
|
static |
|
static |
|
inline |
|
static |
|
inline |
|
static |
|
inline |
::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 | ) |