TT-MLIR
Classes | Namespaces | Enumerations | Functions | Variables
program_generated.h File Reference
#include "flatbuffers/flatbuffers.h"
#include "types_generated.h"

Go to the source code of this file.

Classes

struct  tt::target::metal::KernelConfigTraits< T >
 
struct  tt::target::metal::KernelConfigTraits< tt::target::metal::NocConfig >
 
struct  tt::target::metal::KernelConfigTraits< tt::target::metal::TensixConfig >
 
struct  tt::target::metal::KernelConfigTraits< tt::target::metal::EthernetConfig >
 
struct  tt::target::metal::KernelTraits< T >
 
struct  tt::target::metal::KernelTraits< tt::target::metal::KernelSource >
 
struct  tt::target::metal::KernelTraits< tt::target::metal::KernelBinary >
 
struct  tt::target::metal::RuntimeArgTraits< T >
 
struct  tt::target::metal::RuntimeArgTraits< tt::target::metal::RuntimeArgTensorAddress >
 
struct  tt::target::metal::RuntimeArgTraits< tt::target::metal::RuntimeArgSemaphoreAddress >
 
struct  tt::target::metal::FLATBUFFERS_FINAL_CLASS
 
struct  tt::target::metal::NocConfigBuilder
 
struct  tt::target::metal::NocConfig::Traits
 
struct  tt::target::metal::TensixConfigBuilder
 
struct  tt::target::metal::TensixConfig::Traits
 
struct  tt::target::metal::EthernetConfigBuilder
 
struct  tt::target::metal::EthernetConfig::Traits
 
struct  tt::target::metal::KernelSourceBuilder
 
struct  tt::target::metal::KernelSource::Traits
 
struct  tt::target::metal::KernelBinaryBuilder
 
struct  tt::target::metal::KernelBinary::Traits
 
struct  tt::target::metal::RuntimeArgTensorAddressBuilder
 
struct  tt::target::metal::RuntimeArgTensorAddress::Traits
 
struct  tt::target::metal::RuntimeArgSemaphoreAddressBuilder
 
struct  tt::target::metal::RuntimeArgSemaphoreAddress::Traits
 
struct  tt::target::metal::KernelDescBuilder
 
struct  tt::target::metal::KernelDesc::Traits
 
struct  tt::target::metal::ProgramDescBuilder
 
struct  tt::target::metal::ProgramDesc::Traits
 

Namespaces

 tt
 
 tt::target
 
 tt::target::metal
 

Enumerations

enum class  tt::target::metal::NocIndex : uint16_t { tt::target::metal::Noc0 = 0 , tt::target::metal::Noc1 = 1 , tt::target::metal::MIN = Noc0 , tt::target::metal::MAX = Noc1 }
 
enum class  tt::target::metal::EthType : uint16_t { tt::target::metal::Sender = 0 , tt::target::metal::Receiver = 1 , tt::target::metal::MIN = Sender , tt::target::metal::MAX = Receiver }
 
enum class  tt::target::metal::UnpackToDestMode : uint8_t { tt::target::metal::UnpackToDestFp32 = 0 , tt::target::metal::Default = 1 , tt::target::metal::MIN = UnpackToDestFp32 , tt::target::metal::MAX = Default }
 
enum class  tt::target::metal::KernelConfig : uint8_t {
  tt::target::metal::NONE = 0 , tt::target::metal::NocConfig = 1 , tt::target::metal::TensixConfig = 2 , tt::target::metal::EthernetConfig = 3 ,
  tt::target::metal::MIN = NONE , tt::target::metal::MAX = EthernetConfig
}
 
enum class  tt::target::metal::BinaryType : uint16_t {
  tt::target::metal::BRISC = 0 , tt::target::metal::NCRISC = 1 , tt::target::metal::TRISC0 = 2 , tt::target::metal::TRISC1 = 3 ,
  tt::target::metal::TRISC2 = 4 , tt::target::metal::ERISC = 5 , tt::target::metal::MIN = BRISC , tt::target::metal::MAX = ERISC
}
 
enum class  tt::target::metal::CoreType : uint16_t { tt::target::metal::WORKER = 0 , tt::target::metal::ETH = 1 , tt::target::metal::MIN = WORKER , tt::target::metal::MAX = ETH }
 
enum class  tt::target::metal::Kernel : uint8_t {
  tt::target::metal::NONE = 0 , tt::target::metal::KernelSource = 1 , tt::target::metal::KernelBinary = 2 , tt::target::metal::MIN = NONE ,
  tt::target::metal::MAX = KernelBinary
}
 
enum class  tt::target::metal::RuntimeArg : uint8_t {
  tt::target::metal::NONE = 0 , tt::target::metal::RuntimeArgTensorAddress = 1 , tt::target::metal::RuntimeArgSemaphoreAddress = 2 , tt::target::metal::MIN = NONE ,
  tt::target::metal::MAX = RuntimeArgSemaphoreAddress
}
 

Functions

const NocIndex(& tt::target::metal::EnumValuesNocIndex ())[2]
 
const char *const * tt::target::metal::EnumNamesNocIndex ()
 
const char * tt::target::metal::EnumNameNocIndex (NocIndex e)
 
const EthType(& tt::target::metal::EnumValuesEthType ())[2]
 
const char *const * tt::target::metal::EnumNamesEthType ()
 
const char * tt::target::metal::EnumNameEthType (EthType e)
 
const UnpackToDestMode(& tt::target::metal::EnumValuesUnpackToDestMode ())[2]
 
const char *const * tt::target::metal::EnumNamesUnpackToDestMode ()
 
const char * tt::target::metal::EnumNameUnpackToDestMode (UnpackToDestMode e)
 
const KernelConfig(& tt::target::metal::EnumValuesKernelConfig ())[4]
 
const char *const * tt::target::metal::EnumNamesKernelConfig ()
 
const char * tt::target::metal::EnumNameKernelConfig (KernelConfig e)
 
bool tt::target::metal::VerifyKernelConfig (::flatbuffers::Verifier &verifier, const void *obj, KernelConfig type)
 
bool tt::target::metal::VerifyKernelConfigVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< KernelConfig > *types)
 
const BinaryType(& tt::target::metal::EnumValuesBinaryType ())[6]
 
const char *const * tt::target::metal::EnumNamesBinaryType ()
 
const char * tt::target::metal::EnumNameBinaryType (BinaryType e)
 
const CoreType(& tt::target::metal::EnumValuesCoreType ())[2]
 
const char *const * tt::target::metal::EnumNamesCoreType ()
 
const char * tt::target::metal::EnumNameCoreType (CoreType e)
 
const Kernel(& tt::target::metal::EnumValuesKernel ())[3]
 
const char *const * tt::target::metal::EnumNamesKernel ()
 
const char * tt::target::metal::EnumNameKernel (Kernel e)
 
bool tt::target::metal::VerifyKernel (::flatbuffers::Verifier &verifier, const void *obj, Kernel type)
 
bool tt::target::metal::VerifyKernelVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< Kernel > *types)
 
const RuntimeArg(& tt::target::metal::EnumValuesRuntimeArg ())[3]
 
const char *const * tt::target::metal::EnumNamesRuntimeArg ()
 
const char * tt::target::metal::EnumNameRuntimeArg (RuntimeArg e)
 
bool tt::target::metal::VerifyRuntimeArg (::flatbuffers::Verifier &verifier, const void *obj, RuntimeArg type)
 
bool tt::target::metal::VerifyRuntimeArgVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< RuntimeArg > *types)
 
inline ::flatbuffers::Offset< NocConfig > tt::target::metal::CreateNocConfig (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::NocIndex noc_index=tt::target::metal::NocIndex::Noc0)
 
inline ::flatbuffers::Offset< TensixConfig > tt::target::metal::CreateTensixConfig (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::MathFidelity math_fidelity=tt::target::MathFidelity::LoFi, bool fp32_dest_acc_en=false, bool math_approx_mode=false, ::flatbuffers::Offset<::flatbuffers::Vector< tt::target::metal::UnpackToDestMode >> unpack_to_dest_mode=0)
 
inline ::flatbuffers::Offset< TensixConfig > tt::target::metal::CreateTensixConfigDirect (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::MathFidelity math_fidelity=tt::target::MathFidelity::LoFi, bool fp32_dest_acc_en=false, bool math_approx_mode=false, const std::vector< tt::target::metal::UnpackToDestMode > *unpack_to_dest_mode=nullptr)
 
inline ::flatbuffers::Offset< EthernetConfig > tt::target::metal::CreateEthernetConfig (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::EthType eth_type=tt::target::metal::EthType::Sender, tt::target::metal::NocIndex noc_index=tt::target::metal::NocIndex::Noc0)
 
template<>
const tt::target::metal::NocConfig * tt::target::metal::KernelSource::config_as< tt::target::metal::NocConfig > () const
 
template<>
const tt::target::metal::TensixConfig * tt::target::metal::KernelSource::config_as< tt::target::metal::TensixConfig > () const
 
template<>
const tt::target::metal::EthernetConfig * tt::target::metal::KernelSource::config_as< tt::target::metal::EthernetConfig > () const
 
inline ::flatbuffers::Offset< KernelSource > tt::target::metal::CreateKernelSource (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::String > source=0, tt::target::metal::KernelConfig config_type=tt::target::metal::KernelConfig::NONE, ::flatbuffers::Offset< void > config=0)
 
inline ::flatbuffers::Offset< KernelSource > tt::target::metal::CreateKernelSourceDirect (::flatbuffers::FlatBufferBuilder &_fbb, const char *source=nullptr, tt::target::metal::KernelConfig config_type=tt::target::metal::KernelConfig::NONE, ::flatbuffers::Offset< void > config=0)
 
inline ::flatbuffers::Offset< KernelBinary > tt::target::metal::CreateKernelBinary (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::BinaryType core_type=tt::target::metal::BinaryType::BRISC, ::flatbuffers::Offset<::flatbuffers::Vector< uint8_t >> data=0, ::flatbuffers::Offset<::flatbuffers::String > debug_source=0)
 
inline ::flatbuffers::Offset< KernelBinary > tt::target::metal::CreateKernelBinaryDirect (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::BinaryType core_type=tt::target::metal::BinaryType::BRISC, const std::vector< uint8_t > *data=nullptr, const char *debug_source=nullptr)
 
inline ::flatbuffers::Offset< RuntimeArgTensorAddress > tt::target::metal::CreateRuntimeArgTensorAddress (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t operand_idx=0)
 
inline ::flatbuffers::Offset< RuntimeArgSemaphoreAddress > tt::target::metal::CreateRuntimeArgSemaphoreAddress (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t initial_value=0, tt::target::metal::CoreType core_type=tt::target::metal::CoreType::WORKER)
 
template<>
const tt::target::metal::KernelSource * tt::target::metal::KernelDesc::kernel_as< tt::target::metal::KernelSource > () const
 
template<>
const tt::target::metal::KernelBinary * tt::target::metal::KernelDesc::kernel_as< tt::target::metal::KernelBinary > () const
 
inline ::flatbuffers::Offset< KernelDesc > tt::target::metal::CreateKernelDesc (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::Kernel kernel_type=tt::target::metal::Kernel::NONE, ::flatbuffers::Offset< void > kernel=0, ::flatbuffers::Offset<::flatbuffers::Vector< const tt::target::Dim2dRange * >> core_range_set=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::CBRef >>> cbs=0, ::flatbuffers::Offset<::flatbuffers::Vector< tt::target::metal::RuntimeArg >> runtime_args_type=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< void >>> runtime_args=0, ::flatbuffers::Offset<::flatbuffers::String > debug_info=0)
 
inline ::flatbuffers::Offset< KernelDesc > tt::target::metal::CreateKernelDescDirect (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::Kernel kernel_type=tt::target::metal::Kernel::NONE, ::flatbuffers::Offset< void > kernel=0, const std::vector< tt::target::Dim2dRange > *core_range_set=nullptr, const std::vector<::flatbuffers::Offset< tt::target::CBRef >> *cbs=nullptr, const std::vector< tt::target::metal::RuntimeArg > *runtime_args_type=nullptr, const std::vector<::flatbuffers::Offset< void >> *runtime_args=nullptr, const char *debug_info=nullptr)
 
inline ::flatbuffers::Offset< ProgramDesc > tt::target::metal::CreateProgramDesc (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::KernelDesc >>> kernels=0)
 
inline ::flatbuffers::Offset< ProgramDesc > tt::target::metal::CreateProgramDescDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector<::flatbuffers::Offset< tt::target::metal::KernelDesc >> *kernels=nullptr)
 

Variables

 VT_MATH_FIDELITY = 4
 
 VT_FP32_DEST_ACC_EN = 6
 
 VT_MATH_APPROX_MODE = 8
 
 VT_ETH_TYPE = 4
 
 VT_SOURCE = 4
 
 VT_CONFIG_TYPE = 6
 
 VT_CORE_TYPE = 4
 
 VT_DATA = 6
 
 VT_INITIAL_VALUE = 4
 
 VT_KERNEL_TYPE = 4
 
 VT_KERNEL = 6
 
 VT_CORE_RANGE_SET = 8
 
 VT_CBS = 10
 
 VT_RUNTIME_ARGS_TYPE = 12
 
 VT_RUNTIME_ARGS = 14
 

Variable Documentation

◆ VT_CBS

VT_CBS = 10

◆ VT_CONFIG_TYPE

VT_CONFIG_TYPE = 6

◆ VT_CORE_RANGE_SET

VT_CORE_RANGE_SET = 8

◆ VT_CORE_TYPE

VT_CORE_TYPE = 4

◆ VT_DATA

VT_DATA = 6

◆ VT_ETH_TYPE

VT_ETH_TYPE = 4

◆ VT_FP32_DEST_ACC_EN

VT_FP32_DEST_ACC_EN = 6

◆ VT_INITIAL_VALUE

VT_INITIAL_VALUE = 4

◆ VT_KERNEL

VT_KERNEL = 6

◆ VT_KERNEL_TYPE

VT_KERNEL_TYPE = 4

◆ VT_MATH_APPROX_MODE

VT_MATH_APPROX_MODE = 8

◆ VT_MATH_FIDELITY

VT_MATH_FIDELITY = 4

◆ VT_RUNTIME_ARGS

VT_RUNTIME_ARGS = 14

◆ VT_RUNTIME_ARGS_TYPE

VT_RUNTIME_ARGS_TYPE = 12

◆ VT_SOURCE

VT_SOURCE = 4