TT-MLIR
Classes | Enumerations | Functions
tt::target::metal Namespace Reference

Classes

struct  TTMetalBinaryBinarySchema
 
struct  FLATBUFFERS_FINAL_CLASS
 
struct  DeviceProgramBuilder
 
struct  ProgramBuilder
 
struct  TTMetalBinaryBuilder
 
struct  HostBufferTraits
 
struct  HostBufferTraits< tt::target::metal::TensorRef >
 
struct  HostBufferTraits< tt::target::metal::ConstantBuffer8 >
 
struct  HostBufferTraits< tt::target::metal::ConstantBuffer16 >
 
struct  HostBufferTraits< tt::target::metal::ConstantBuffer32 >
 
struct  CommandTypeTraits
 
struct  CommandTypeTraits< tt::target::metal::EnqueueProgramCommand >
 
struct  CommandTypeTraits< tt::target::metal::EnqueueWriteBufferCommand >
 
struct  CommandTypeTraits< tt::target::metal::EnqueueReadBufferCommand >
 
struct  CommandTypeTraits< tt::target::metal::CreateBufferCommand >
 
struct  CommandTypeTraits< tt::target::metal::DeallocateBufferCommand >
 
struct  CommandTypeTraits< tt::target::metal::CreateEventCommand >
 
struct  CommandTypeTraits< tt::target::metal::EnqueueRecordEventCommand >
 
struct  CommandTypeTraits< tt::target::metal::EnqueueWaitForEventCommand >
 
struct  CommandTypeTraits< tt::target::metal::EventSynchronizeCommand >
 
struct  CommandTypeTraits< tt::target::metal::EventQueryCommand >
 
struct  CommandTypeTraits< tt::target::metal::FinishCommand >
 
struct  EnqueueProgramCommandBuilder
 
struct  ConstantBuffer8Builder
 
struct  ConstantBuffer16Builder
 
struct  ConstantBuffer32Builder
 
struct  EnqueueWriteBufferCommandBuilder
 
struct  EnqueueReadBufferCommandBuilder
 
struct  CreateBufferCommandBuilder
 
struct  DeallocateBufferCommandBuilder
 
struct  CreateEventCommandBuilder
 
struct  EnqueueRecordEventCommandBuilder
 
struct  EnqueueWaitForEventCommandBuilder
 
struct  EventSynchronizeCommandBuilder
 
struct  EventQueryCommandBuilder
 
struct  FinishCommandBuilder
 
struct  CommandBuilder
 
struct  CommandQueueBuilder
 
struct  KernelConfigTraits
 
struct  KernelConfigTraits< tt::target::metal::NocConfig >
 
struct  KernelConfigTraits< tt::target::metal::TensixConfig >
 
struct  KernelConfigTraits< tt::target::metal::EthernetConfig >
 
struct  KernelTraits
 
struct  KernelTraits< tt::target::metal::KernelSource >
 
struct  KernelTraits< tt::target::metal::KernelBinary >
 
struct  RuntimeArgTraits
 
struct  RuntimeArgTraits< tt::target::metal::RuntimeArgTensorAddress >
 
struct  RuntimeArgTraits< tt::target::metal::RuntimeArgSemaphoreAddress >
 
struct  NocConfigBuilder
 
struct  TensixConfigBuilder
 
struct  EthernetConfigBuilder
 
struct  KernelSourceBuilder
 
struct  KernelBinaryBuilder
 
struct  RuntimeArgTensorAddressBuilder
 
struct  RuntimeArgSemaphoreAddressBuilder
 
struct  KernelDescBuilder
 
struct  ProgramDescBuilder
 
struct  MemoryDescBuilder
 
struct  LayoutDescBuilder
 
struct  TensorDescBuilder
 
struct  CBDescBuilder
 
struct  TensorRefBuilder
 
struct  CBRefBuilder
 

Enumerations

enum class  HostBuffer : uint8_t {
  NONE = 0 , TensorRef = 1 , ConstantBuffer8 = 2 , ConstantBuffer16 = 3 ,
  ConstantBuffer32 = 4 , MIN = NONE , MAX = ConstantBuffer32
}
 
enum class  CommandType : uint8_t {
  NONE = 0 , EnqueueProgramCommand = 1 , EnqueueWriteBufferCommand = 2 , EnqueueReadBufferCommand = 3 ,
  CreateBufferCommand = 4 , DeallocateBufferCommand = 5 , CreateEventCommand = 6 , EnqueueRecordEventCommand = 7 ,
  EnqueueWaitForEventCommand = 8 , EventSynchronizeCommand = 9 , EventQueryCommand = 10 , FinishCommand = 11 ,
  MIN = NONE , MAX = FinishCommand
}
 
enum class  NocIndex : uint16_t { Noc0 = 0 , Noc1 = 1 , MIN = Noc0 , MAX = Noc1 }
 
enum class  EthType : uint16_t { Sender = 0 , Receiver = 1 , MIN = Sender , MAX = Receiver }
 
enum class  UnpackToDestMode : uint8_t { UnpackToDestFp32 = 0 , Default = 1 , MIN = UnpackToDestFp32 , MAX = Default }
 
enum class  KernelConfig : uint8_t {
  NONE = 0 , NocConfig = 1 , TensixConfig = 2 , EthernetConfig = 3 ,
  MIN = NONE , MAX = EthernetConfig
}
 
enum class  BinaryType : uint16_t {
  BRISC = 0 , NCRISC = 1 , TRISC0 = 2 , TRISC1 = 3 ,
  TRISC2 = 4 , ERISC = 5 , MIN = BRISC , MAX = ERISC
}
 
enum class  CoreType : uint16_t { WORKER = 0 , ETH = 1 , MIN = WORKER , MAX = ETH }
 
enum class  Kernel : uint8_t {
  NONE = 0 , KernelSource = 1 , KernelBinary = 2 , MIN = NONE ,
  MAX = KernelBinary
}
 
enum class  RuntimeArg : uint8_t {
  NONE = 0 , RuntimeArgTensorAddress = 1 , RuntimeArgSemaphoreAddress = 2 , MIN = NONE ,
  MAX = RuntimeArgSemaphoreAddress
}
 

Functions

inline ::flatbuffers::Offset< DeviceProgram > CreateDeviceProgram (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>> inputs=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>> outputs=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::CommandQueue >>> command_queues=0)
 
inline ::flatbuffers::Offset< DeviceProgram > CreateDeviceProgramDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *inputs=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *outputs=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::CommandQueue >> *command_queues=nullptr)
 
inline ::flatbuffers::Offset< Program > CreateProgram (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::String > name=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>> inputs=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>> outputs=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::DeviceProgram >>> device_programs=0, ::flatbuffers::Offset< tt::target::DebugInfo > debug_info=0)
 
inline ::flatbuffers::Offset< Program > CreateProgramDirect (::flatbuffers::FlatBufferBuilder &_fbb, const char *name=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *inputs=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *outputs=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::DeviceProgram >> *device_programs=nullptr, ::flatbuffers::Offset< tt::target::DebugInfo > debug_info=0)
 
inline ::flatbuffers::Offset< TTMetalBinary > CreateTTMetalBinary (::flatbuffers::FlatBufferBuilder &_fbb, const tt::target::Version *version=nullptr, ::flatbuffers::Offset<::flatbuffers::String > ttmlir_git_hash=0, ::flatbuffers::Offset< tt::target::SystemDesc > system_desc=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::Program >>> programs=0)
 
inline ::flatbuffers::Offset< TTMetalBinary > CreateTTMetalBinaryDirect (::flatbuffers::FlatBufferBuilder &_fbb, const tt::target::Version *version=nullptr, const char *ttmlir_git_hash=nullptr, ::flatbuffers::Offset< tt::target::SystemDesc > system_desc=0, const std::vector<::flatbuffers::Offset< tt::target::metal::Program >> *programs=nullptr)
 
const tt::target::metal::TTMetalBinary * GetTTMetalBinary (const void *buf)
 
const tt::target::metal::TTMetalBinary * GetSizePrefixedTTMetalBinary (const void *buf)
 
const char * TTMetalBinaryIdentifier ()
 
bool TTMetalBinaryBufferHasIdentifier (const void *buf)
 
bool SizePrefixedTTMetalBinaryBufferHasIdentifier (const void *buf)
 
bool VerifyTTMetalBinaryBuffer (::flatbuffers::Verifier &verifier)
 
bool VerifySizePrefixedTTMetalBinaryBuffer (::flatbuffers::Verifier &verifier)
 
const char * TTMetalBinaryExtension ()
 
void FinishTTMetalBinaryBuffer (::flatbuffers::FlatBufferBuilder &fbb, ::flatbuffers::Offset< tt::target::metal::TTMetalBinary > root)
 
void FinishSizePrefixedTTMetalBinaryBuffer (::flatbuffers::FlatBufferBuilder &fbb, ::flatbuffers::Offset< tt::target::metal::TTMetalBinary > root)
 
const HostBuffer(& EnumValuesHostBuffer ())[5]
 
const char *const * EnumNamesHostBuffer ()
 
const char * EnumNameHostBuffer (HostBuffer e)
 
bool VerifyHostBuffer (::flatbuffers::Verifier &verifier, const void *obj, HostBuffer type)
 
bool VerifyHostBufferVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< HostBuffer > *types)
 
const CommandType(& EnumValuesCommandType ())[12]
 
const char *const * EnumNamesCommandType ()
 
const char * EnumNameCommandType (CommandType e)
 
bool VerifyCommandType (::flatbuffers::Verifier &verifier, const void *obj, CommandType type)
 
bool VerifyCommandTypeVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< CommandType > *types)
 
inline ::flatbuffers::Offset< EnqueueProgramCommand > CreateEnqueueProgramCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>> operands=0, ::flatbuffers::Offset< tt::target::metal::ProgramDesc > program=0)
 
inline ::flatbuffers::Offset< EnqueueProgramCommand > CreateEnqueueProgramCommandDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *operands=nullptr, ::flatbuffers::Offset< tt::target::metal::ProgramDesc > program=0)
 
inline ::flatbuffers::Offset< ConstantBuffer8 > CreateConstantBuffer8 (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector< uint8_t >> data=0)
 
inline ::flatbuffers::Offset< ConstantBuffer8 > CreateConstantBuffer8Direct (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector< uint8_t > *data=nullptr)
 
inline ::flatbuffers::Offset< ConstantBuffer16 > CreateConstantBuffer16 (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector< uint16_t >> data=0)
 
inline ::flatbuffers::Offset< ConstantBuffer16 > CreateConstantBuffer16Direct (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector< uint16_t > *data=nullptr)
 
inline ::flatbuffers::Offset< ConstantBuffer32 > CreateConstantBuffer32 (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector< uint32_t >> data=0)
 
inline ::flatbuffers::Offset< ConstantBuffer32 > CreateConstantBuffer32Direct (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector< uint32_t > *data=nullptr)
 
template<>
const tt::target::metal::TensorRef * EnqueueWriteBufferCommand::src_as< tt::target::metal::TensorRef > () const
 
template<>
const tt::target::metal::ConstantBuffer8 * EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer8 > () const
 
template<>
const tt::target::metal::ConstantBuffer16 * EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer16 > () const
 
template<>
const tt::target::metal::ConstantBuffer32 * EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer32 > () const
 
inline ::flatbuffers::Offset< EnqueueWriteBufferCommand > CreateEnqueueWriteBufferCommand (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::HostBuffer src_type=tt::target::metal::HostBuffer::NONE, ::flatbuffers::Offset< void > src=0, ::flatbuffers::Offset< tt::target::metal::TensorRef > dst=0)
 
inline ::flatbuffers::Offset< EnqueueReadBufferCommand > CreateEnqueueReadBufferCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::TensorRef > src=0, ::flatbuffers::Offset< tt::target::metal::TensorRef > dst=0)
 
inline ::flatbuffers::Offset< CreateBufferCommand > CreateCreateBufferCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::TensorRef > ref=0)
 
inline ::flatbuffers::Offset< DeallocateBufferCommand > CreateDeallocateBufferCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::TensorRef > ref=0)
 
inline ::flatbuffers::Offset< CreateEventCommand > CreateCreateEventCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::EventRef > ref=0)
 
inline ::flatbuffers::Offset< EnqueueRecordEventCommand > CreateEnqueueRecordEventCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::EventRef > ref=0)
 
inline ::flatbuffers::Offset< EnqueueWaitForEventCommand > CreateEnqueueWaitForEventCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::EventRef > ref=0)
 
inline ::flatbuffers::Offset< EventSynchronizeCommand > CreateEventSynchronizeCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::EventRef > ref=0)
 
inline ::flatbuffers::Offset< EventQueryCommand > CreateEventQueryCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::EventRef > ref=0)
 
inline ::flatbuffers::Offset< FinishCommand > CreateFinishCommand (::flatbuffers::FlatBufferBuilder &_fbb)
 
template<>
const tt::target::metal::EnqueueProgramCommand * Command::type_as< tt::target::metal::EnqueueProgramCommand > () const
 
template<>
const tt::target::metal::EnqueueWriteBufferCommand * Command::type_as< tt::target::metal::EnqueueWriteBufferCommand > () const
 
template<>
const tt::target::metal::EnqueueReadBufferCommand * Command::type_as< tt::target::metal::EnqueueReadBufferCommand > () const
 
template<>
const tt::target::metal::CreateBufferCommand * Command::type_as< tt::target::metal::CreateBufferCommand > () const
 
template<>
const tt::target::metal::DeallocateBufferCommand * Command::type_as< tt::target::metal::DeallocateBufferCommand > () const
 
template<>
const tt::target::metal::CreateEventCommand * Command::type_as< tt::target::metal::CreateEventCommand > () const
 
template<>
const tt::target::metal::EnqueueRecordEventCommand * Command::type_as< tt::target::metal::EnqueueRecordEventCommand > () const
 
template<>
const tt::target::metal::EnqueueWaitForEventCommand * Command::type_as< tt::target::metal::EnqueueWaitForEventCommand > () const
 
template<>
const tt::target::metal::EventSynchronizeCommand * Command::type_as< tt::target::metal::EventSynchronizeCommand > () const
 
template<>
const tt::target::metal::EventQueryCommand * Command::type_as< tt::target::metal::EventQueryCommand > () const
 
template<>
const tt::target::metal::FinishCommand * Command::type_as< tt::target::metal::FinishCommand > () const
 
inline ::flatbuffers::Offset< Command > CreateCommand (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::CommandType type_type=tt::target::metal::CommandType::NONE, ::flatbuffers::Offset< void > type=0, ::flatbuffers::Offset<::flatbuffers::String > debug_info=0)
 
inline ::flatbuffers::Offset< Command > CreateCommandDirect (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::CommandType type_type=tt::target::metal::CommandType::NONE, ::flatbuffers::Offset< void > type=0, const char *debug_info=nullptr)
 
inline ::flatbuffers::Offset< CommandQueue > CreateCommandQueue (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::String > name=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::Command >>> commands=0)
 
inline ::flatbuffers::Offset< CommandQueue > CreateCommandQueueDirect (::flatbuffers::FlatBufferBuilder &_fbb, const char *name=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::Command >> *commands=nullptr)
 
const NocIndex(& EnumValuesNocIndex ())[2]
 
const char *const * EnumNamesNocIndex ()
 
const char * EnumNameNocIndex (NocIndex e)
 
const EthType(& EnumValuesEthType ())[2]
 
const char *const * EnumNamesEthType ()
 
const char * EnumNameEthType (EthType e)
 
const UnpackToDestMode(& EnumValuesUnpackToDestMode ())[2]
 
const char *const * EnumNamesUnpackToDestMode ()
 
const char * EnumNameUnpackToDestMode (UnpackToDestMode e)
 
const KernelConfig(& EnumValuesKernelConfig ())[4]
 
const char *const * EnumNamesKernelConfig ()
 
const char * EnumNameKernelConfig (KernelConfig e)
 
bool VerifyKernelConfig (::flatbuffers::Verifier &verifier, const void *obj, KernelConfig type)
 
bool VerifyKernelConfigVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< KernelConfig > *types)
 
const BinaryType(& EnumValuesBinaryType ())[6]
 
const char *const * EnumNamesBinaryType ()
 
const char * EnumNameBinaryType (BinaryType e)
 
const CoreType(& EnumValuesCoreType ())[2]
 
const char *const * EnumNamesCoreType ()
 
const char * EnumNameCoreType (CoreType e)
 
const Kernel(& EnumValuesKernel ())[3]
 
const char *const * EnumNamesKernel ()
 
const char * EnumNameKernel (Kernel e)
 
bool VerifyKernel (::flatbuffers::Verifier &verifier, const void *obj, Kernel type)
 
bool VerifyKernelVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< Kernel > *types)
 
const RuntimeArg(& EnumValuesRuntimeArg ())[3]
 
const char *const * EnumNamesRuntimeArg ()
 
const char * EnumNameRuntimeArg (RuntimeArg e)
 
bool VerifyRuntimeArg (::flatbuffers::Verifier &verifier, const void *obj, RuntimeArg type)
 
bool VerifyRuntimeArgVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< RuntimeArg > *types)
 
inline ::flatbuffers::Offset< NocConfig > CreateNocConfig (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::NocIndex noc_index=tt::target::metal::NocIndex::Noc0)
 
inline ::flatbuffers::Offset< TensixConfig > 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 > 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 > 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 * KernelSource::config_as< tt::target::metal::NocConfig > () const
 
template<>
const tt::target::metal::TensixConfig * KernelSource::config_as< tt::target::metal::TensixConfig > () const
 
template<>
const tt::target::metal::EthernetConfig * KernelSource::config_as< tt::target::metal::EthernetConfig > () const
 
inline ::flatbuffers::Offset< KernelSource > 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 > 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 > 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 > 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 > CreateRuntimeArgTensorAddress (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t operand_idx=0)
 
inline ::flatbuffers::Offset< RuntimeArgSemaphoreAddress > 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 * KernelDesc::kernel_as< tt::target::metal::KernelSource > () const
 
template<>
const tt::target::metal::KernelBinary * KernelDesc::kernel_as< tt::target::metal::KernelBinary > () const
 
inline ::flatbuffers::Offset< KernelDesc > 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::metal::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 > 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::metal::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 > CreateProgramDesc (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::KernelDesc >>> kernels=0)
 
inline ::flatbuffers::Offset< ProgramDesc > CreateProgramDescDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector<::flatbuffers::Offset< tt::target::metal::KernelDesc >> *kernels=nullptr)
 
inline ::flatbuffers::Offset< MemoryDesc > CreateMemoryDesc (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector< int32_t >> shape=0, const tt::target::Dim2d *tile_shape=nullptr, tt::target::DataType data_type=tt::target::DataType::Float32, tt::target::MemorySpace memory_space=tt::target::MemorySpace::System, uint64_t size=0)
 
inline ::flatbuffers::Offset< MemoryDesc > CreateMemoryDescDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector< int32_t > *shape=nullptr, const tt::target::Dim2d *tile_shape=nullptr, tt::target::DataType data_type=tt::target::DataType::Float32, tt::target::MemorySpace memory_space=tt::target::MemorySpace::System, uint64_t size=0)
 
inline ::flatbuffers::Offset< LayoutDesc > CreateLayoutDesc (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::OOBVal oob_val=tt::target::OOBVal::Undef, ::flatbuffers::Offset<::flatbuffers::Vector< const tt::target::Dim2dRange * >> core_range_set=0, ::flatbuffers::Offset< tt::target::metal::MemoryDesc > memory_desc=0)
 
inline ::flatbuffers::Offset< LayoutDesc > CreateLayoutDescDirect (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::OOBVal oob_val=tt::target::OOBVal::Undef, const std::vector< tt::target::Dim2dRange > *core_range_set=nullptr, ::flatbuffers::Offset< tt::target::metal::MemoryDesc > memory_desc=0)
 
inline ::flatbuffers::Offset< TensorDesc > CreateTensorDesc (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector< int32_t >> shape=0, ::flatbuffers::Offset< tt::target::metal::LayoutDesc > layout=0)
 
inline ::flatbuffers::Offset< TensorDesc > CreateTensorDescDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector< int32_t > *shape=nullptr, ::flatbuffers::Offset< tt::target::metal::LayoutDesc > layout=0)
 
inline ::flatbuffers::Offset< CBDesc > CreateCBDesc (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t port=0, ::flatbuffers::Offset< tt::target::metal::MemoryDesc > memory_desc=0, uint64_t page_size=0, uint64_t num_buffers=0)
 
inline ::flatbuffers::Offset< TensorRef > CreateTensorRef (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t global_id=0, uint64_t address=0, uint64_t size=0, ::flatbuffers::Offset< tt::target::metal::TensorDesc > desc=0)
 
inline ::flatbuffers::Offset< CBRef > CreateCBRef (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t global_id=0, ::flatbuffers::Offset< tt::target::metal::TensorRef > tensor_ref=0, uint64_t address=0, ::flatbuffers::Offset< tt::target::metal::CBDesc > desc=0)
 

Enumeration Type Documentation

◆ BinaryType

enum tt::target::metal::BinaryType : uint16_t
strong
Enumerator
BRISC 
NCRISC 
TRISC0 
TRISC1 
TRISC2 
ERISC 
MIN 
MAX 

◆ CommandType

enum tt::target::metal::CommandType : uint8_t
strong
Enumerator
NONE 
EnqueueProgramCommand 
EnqueueWriteBufferCommand 
EnqueueReadBufferCommand 
CreateBufferCommand 
DeallocateBufferCommand 
CreateEventCommand 
EnqueueRecordEventCommand 
EnqueueWaitForEventCommand 
EventSynchronizeCommand 
EventQueryCommand 
FinishCommand 
MIN 
MAX 

◆ CoreType

enum tt::target::metal::CoreType : uint16_t
strong
Enumerator
WORKER 
ETH 
MIN 
MAX 

◆ EthType

enum tt::target::metal::EthType : uint16_t
strong
Enumerator
Sender 
Receiver 
MIN 
MAX 

◆ HostBuffer

enum tt::target::metal::HostBuffer : uint8_t
strong
Enumerator
NONE 
TensorRef 
ConstantBuffer8 
ConstantBuffer16 
ConstantBuffer32 
MIN 
MAX 

◆ Kernel

enum tt::target::metal::Kernel : uint8_t
strong
Enumerator
NONE 
KernelSource 
KernelBinary 
MIN 
MAX 

◆ KernelConfig

enum tt::target::metal::KernelConfig : uint8_t
strong
Enumerator
NONE 
NocConfig 
TensixConfig 
EthernetConfig 
MIN 
MAX 

◆ NocIndex

enum tt::target::metal::NocIndex : uint16_t
strong
Enumerator
Noc0 
Noc1 
MIN 
MAX 

◆ RuntimeArg

enum tt::target::metal::RuntimeArg : uint8_t
strong
Enumerator
NONE 
RuntimeArgTensorAddress 
RuntimeArgSemaphoreAddress 
MIN 
MAX 

◆ UnpackToDestMode

enum tt::target::metal::UnpackToDestMode : uint8_t
strong
Enumerator
UnpackToDestFp32 
Default 
MIN 
MAX 

Function Documentation

◆ Command::type_as< tt::target::metal::CreateBufferCommand >()

template<>
const tt::target::metal::CreateBufferCommand* tt::target::metal::Command::type_as< tt::target::metal::CreateBufferCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::CreateEventCommand >()

template<>
const tt::target::metal::CreateEventCommand* tt::target::metal::Command::type_as< tt::target::metal::CreateEventCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::DeallocateBufferCommand >()

template<>
const tt::target::metal::DeallocateBufferCommand* tt::target::metal::Command::type_as< tt::target::metal::DeallocateBufferCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::EnqueueProgramCommand >()

template<>
const tt::target::metal::EnqueueProgramCommand* tt::target::metal::Command::type_as< tt::target::metal::EnqueueProgramCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::EnqueueReadBufferCommand >()

template<>
const tt::target::metal::EnqueueReadBufferCommand* tt::target::metal::Command::type_as< tt::target::metal::EnqueueReadBufferCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::EnqueueRecordEventCommand >()

template<>
const tt::target::metal::EnqueueRecordEventCommand* tt::target::metal::Command::type_as< tt::target::metal::EnqueueRecordEventCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::EnqueueWaitForEventCommand >()

template<>
const tt::target::metal::EnqueueWaitForEventCommand* tt::target::metal::Command::type_as< tt::target::metal::EnqueueWaitForEventCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::EnqueueWriteBufferCommand >()

template<>
const tt::target::metal::EnqueueWriteBufferCommand* tt::target::metal::Command::type_as< tt::target::metal::EnqueueWriteBufferCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::EventQueryCommand >()

template<>
const tt::target::metal::EventQueryCommand* tt::target::metal::Command::type_as< tt::target::metal::EventQueryCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::EventSynchronizeCommand >()

template<>
const tt::target::metal::EventSynchronizeCommand* tt::target::metal::Command::type_as< tt::target::metal::EventSynchronizeCommand > ( ) const
inline

◆ Command::type_as< tt::target::metal::FinishCommand >()

template<>
const tt::target::metal::FinishCommand* tt::target::metal::Command::type_as< tt::target::metal::FinishCommand > ( ) const
inline

◆ CreateCBDesc()

inline ::flatbuffers::Offset<CBDesc> tt::target::metal::CreateCBDesc ( ::flatbuffers::FlatBufferBuilder &  _fbb,
uint32_t  port = 0,
::flatbuffers::Offset< tt::target::metal::MemoryDesc >  memory_desc = 0,
uint64_t  page_size = 0,
uint64_t  num_buffers = 0 
)

◆ CreateCBRef()

inline ::flatbuffers::Offset<CBRef> tt::target::metal::CreateCBRef ( ::flatbuffers::FlatBufferBuilder &  _fbb,
uint32_t  global_id = 0,
::flatbuffers::Offset< tt::target::metal::TensorRef >  tensor_ref = 0,
uint64_t  address = 0,
::flatbuffers::Offset< tt::target::metal::CBDesc >  desc = 0 
)

◆ CreateCommand()

inline ::flatbuffers::Offset<Command> tt::target::metal::CreateCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
tt::target::metal::CommandType  type_type = tt::target::metal::CommandType::NONE,
::flatbuffers::Offset< void >  type = 0,
::flatbuffers::Offset<::flatbuffers::String >  debug_info = 0 
)

◆ CreateCommandDirect()

inline ::flatbuffers::Offset<Command> tt::target::metal::CreateCommandDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
tt::target::metal::CommandType  type_type = tt::target::metal::CommandType::NONE,
::flatbuffers::Offset< void >  type = 0,
const char *  debug_info = nullptr 
)

◆ CreateCommandQueue()

inline ::flatbuffers::Offset<CommandQueue> tt::target::metal::CreateCommandQueue ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::String >  name = 0,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::Command >>>  commands = 0 
)

◆ CreateCommandQueueDirect()

inline ::flatbuffers::Offset<CommandQueue> tt::target::metal::CreateCommandQueueDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const char *  name = nullptr,
const std::vector<::flatbuffers::Offset< tt::target::metal::Command >> *  commands = nullptr 
)

◆ CreateConstantBuffer16()

inline ::flatbuffers::Offset<ConstantBuffer16> tt::target::metal::CreateConstantBuffer16 ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::Vector< uint16_t >>  data = 0 
)

◆ CreateConstantBuffer16Direct()

inline ::flatbuffers::Offset<ConstantBuffer16> tt::target::metal::CreateConstantBuffer16Direct ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const std::vector< uint16_t > *  data = nullptr 
)

◆ CreateConstantBuffer32()

inline ::flatbuffers::Offset<ConstantBuffer32> tt::target::metal::CreateConstantBuffer32 ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::Vector< uint32_t >>  data = 0 
)

◆ CreateConstantBuffer32Direct()

inline ::flatbuffers::Offset<ConstantBuffer32> tt::target::metal::CreateConstantBuffer32Direct ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const std::vector< uint32_t > *  data = nullptr 
)

◆ CreateConstantBuffer8()

inline ::flatbuffers::Offset<ConstantBuffer8> tt::target::metal::CreateConstantBuffer8 ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::Vector< uint8_t >>  data = 0 
)

◆ CreateConstantBuffer8Direct()

inline ::flatbuffers::Offset<ConstantBuffer8> tt::target::metal::CreateConstantBuffer8Direct ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const std::vector< uint8_t > *  data = nullptr 
)

◆ CreateCreateBufferCommand()

inline ::flatbuffers::Offset<CreateBufferCommand> tt::target::metal::CreateCreateBufferCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset< tt::target::metal::TensorRef >  ref = 0 
)

◆ CreateCreateEventCommand()

inline ::flatbuffers::Offset<CreateEventCommand> tt::target::metal::CreateCreateEventCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset< tt::target::EventRef >  ref = 0 
)

◆ CreateDeallocateBufferCommand()

inline ::flatbuffers::Offset<DeallocateBufferCommand> tt::target::metal::CreateDeallocateBufferCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset< tt::target::metal::TensorRef >  ref = 0 
)

◆ CreateDeviceProgram()

inline ::flatbuffers::Offset<DeviceProgram> tt::target::metal::CreateDeviceProgram ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>>  inputs = 0,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>>  outputs = 0,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::CommandQueue >>>  command_queues = 0 
)

◆ CreateDeviceProgramDirect()

inline ::flatbuffers::Offset<DeviceProgram> tt::target::metal::CreateDeviceProgramDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *  inputs = nullptr,
const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *  outputs = nullptr,
const std::vector<::flatbuffers::Offset< tt::target::metal::CommandQueue >> *  command_queues = nullptr 
)

◆ CreateEnqueueProgramCommand()

inline ::flatbuffers::Offset<EnqueueProgramCommand> tt::target::metal::CreateEnqueueProgramCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>>  operands = 0,
::flatbuffers::Offset< tt::target::metal::ProgramDesc >  program = 0 
)

◆ CreateEnqueueProgramCommandDirect()

inline ::flatbuffers::Offset<EnqueueProgramCommand> tt::target::metal::CreateEnqueueProgramCommandDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *  operands = nullptr,
::flatbuffers::Offset< tt::target::metal::ProgramDesc >  program = 0 
)

◆ CreateEnqueueReadBufferCommand()

inline ::flatbuffers::Offset<EnqueueReadBufferCommand> tt::target::metal::CreateEnqueueReadBufferCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset< tt::target::metal::TensorRef >  src = 0,
::flatbuffers::Offset< tt::target::metal::TensorRef >  dst = 0 
)

◆ CreateEnqueueRecordEventCommand()

inline ::flatbuffers::Offset<EnqueueRecordEventCommand> tt::target::metal::CreateEnqueueRecordEventCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset< tt::target::EventRef >  ref = 0 
)

◆ CreateEnqueueWaitForEventCommand()

inline ::flatbuffers::Offset<EnqueueWaitForEventCommand> tt::target::metal::CreateEnqueueWaitForEventCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset< tt::target::EventRef >  ref = 0 
)

◆ CreateEnqueueWriteBufferCommand()

inline ::flatbuffers::Offset<EnqueueWriteBufferCommand> tt::target::metal::CreateEnqueueWriteBufferCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
tt::target::metal::HostBuffer  src_type = tt::target::metal::HostBuffer::NONE,
::flatbuffers::Offset< void >  src = 0,
::flatbuffers::Offset< tt::target::metal::TensorRef >  dst = 0 
)

◆ CreateEthernetConfig()

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 
)

◆ CreateEventQueryCommand()

inline ::flatbuffers::Offset<EventQueryCommand> tt::target::metal::CreateEventQueryCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset< tt::target::EventRef >  ref = 0 
)

◆ CreateEventSynchronizeCommand()

inline ::flatbuffers::Offset<EventSynchronizeCommand> tt::target::metal::CreateEventSynchronizeCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset< tt::target::EventRef >  ref = 0 
)

◆ CreateFinishCommand()

inline ::flatbuffers::Offset<FinishCommand> tt::target::metal::CreateFinishCommand ( ::flatbuffers::FlatBufferBuilder &  _fbb)

◆ CreateKernelBinary()

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 
)

◆ CreateKernelBinaryDirect()

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 
)

◆ CreateKernelDesc()

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::metal::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 
)

◆ CreateKernelDescDirect()

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::metal::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 
)

◆ CreateKernelSource()

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 
)

◆ CreateKernelSourceDirect()

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 
)

◆ CreateLayoutDesc()

inline ::flatbuffers::Offset<LayoutDesc> tt::target::metal::CreateLayoutDesc ( ::flatbuffers::FlatBufferBuilder &  _fbb,
tt::target::OOBVal  oob_val = tt::target::OOBVal::Undef,
::flatbuffers::Offset<::flatbuffers::Vector< const tt::target::Dim2dRange * >>  core_range_set = 0,
::flatbuffers::Offset< tt::target::metal::MemoryDesc >  memory_desc = 0 
)

◆ CreateLayoutDescDirect()

inline ::flatbuffers::Offset<LayoutDesc> tt::target::metal::CreateLayoutDescDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
tt::target::OOBVal  oob_val = tt::target::OOBVal::Undef,
const std::vector< tt::target::Dim2dRange > *  core_range_set = nullptr,
::flatbuffers::Offset< tt::target::metal::MemoryDesc >  memory_desc = 0 
)

◆ CreateMemoryDesc()

inline ::flatbuffers::Offset<MemoryDesc> tt::target::metal::CreateMemoryDesc ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::Vector< int32_t >>  shape = 0,
const tt::target::Dim2d *  tile_shape = nullptr,
tt::target::DataType  data_type = tt::target::DataType::Float32,
tt::target::MemorySpace  memory_space = tt::target::MemorySpace::System,
uint64_t  size = 0 
)

◆ CreateMemoryDescDirect()

inline ::flatbuffers::Offset<MemoryDesc> tt::target::metal::CreateMemoryDescDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const std::vector< int32_t > *  shape = nullptr,
const tt::target::Dim2d *  tile_shape = nullptr,
tt::target::DataType  data_type = tt::target::DataType::Float32,
tt::target::MemorySpace  memory_space = tt::target::MemorySpace::System,
uint64_t  size = 0 
)

◆ CreateNocConfig()

inline ::flatbuffers::Offset<NocConfig> tt::target::metal::CreateNocConfig ( ::flatbuffers::FlatBufferBuilder &  _fbb,
tt::target::metal::NocIndex  noc_index = tt::target::metal::NocIndex::Noc0 
)

◆ CreateProgram()

inline ::flatbuffers::Offset<Program> tt::target::metal::CreateProgram ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::String >  name = 0,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>>  inputs = 0,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::TensorRef >>>  outputs = 0,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::DeviceProgram >>>  device_programs = 0,
::flatbuffers::Offset< tt::target::DebugInfo >  debug_info = 0 
)

◆ CreateProgramDesc()

inline ::flatbuffers::Offset<ProgramDesc> tt::target::metal::CreateProgramDesc ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::KernelDesc >>>  kernels = 0 
)

◆ CreateProgramDescDirect()

inline ::flatbuffers::Offset<ProgramDesc> tt::target::metal::CreateProgramDescDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const std::vector<::flatbuffers::Offset< tt::target::metal::KernelDesc >> *  kernels = nullptr 
)

◆ CreateProgramDirect()

inline ::flatbuffers::Offset<Program> tt::target::metal::CreateProgramDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const char *  name = nullptr,
const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *  inputs = nullptr,
const std::vector<::flatbuffers::Offset< tt::target::metal::TensorRef >> *  outputs = nullptr,
const std::vector<::flatbuffers::Offset< tt::target::metal::DeviceProgram >> *  device_programs = nullptr,
::flatbuffers::Offset< tt::target::DebugInfo >  debug_info = 0 
)

◆ CreateRuntimeArgSemaphoreAddress()

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 
)

◆ CreateRuntimeArgTensorAddress()

inline ::flatbuffers::Offset<RuntimeArgTensorAddress> tt::target::metal::CreateRuntimeArgTensorAddress ( ::flatbuffers::FlatBufferBuilder &  _fbb,
uint32_t  operand_idx = 0 
)

◆ CreateTensixConfig()

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 
)

◆ CreateTensixConfigDirect()

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 
)

◆ CreateTensorDesc()

inline ::flatbuffers::Offset<TensorDesc> tt::target::metal::CreateTensorDesc ( ::flatbuffers::FlatBufferBuilder &  _fbb,
::flatbuffers::Offset<::flatbuffers::Vector< int32_t >>  shape = 0,
::flatbuffers::Offset< tt::target::metal::LayoutDesc >  layout = 0 
)

◆ CreateTensorDescDirect()

inline ::flatbuffers::Offset<TensorDesc> tt::target::metal::CreateTensorDescDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const std::vector< int32_t > *  shape = nullptr,
::flatbuffers::Offset< tt::target::metal::LayoutDesc >  layout = 0 
)

◆ CreateTensorRef()

inline ::flatbuffers::Offset<TensorRef> tt::target::metal::CreateTensorRef ( ::flatbuffers::FlatBufferBuilder &  _fbb,
uint32_t  global_id = 0,
uint64_t  address = 0,
uint64_t  size = 0,
::flatbuffers::Offset< tt::target::metal::TensorDesc >  desc = 0 
)

◆ CreateTTMetalBinary()

inline ::flatbuffers::Offset<TTMetalBinary> tt::target::metal::CreateTTMetalBinary ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const tt::target::Version *  version = nullptr,
::flatbuffers::Offset<::flatbuffers::String >  ttmlir_git_hash = 0,
::flatbuffers::Offset< tt::target::SystemDesc >  system_desc = 0,
::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::Program >>>  programs = 0 
)

◆ CreateTTMetalBinaryDirect()

inline ::flatbuffers::Offset<TTMetalBinary> tt::target::metal::CreateTTMetalBinaryDirect ( ::flatbuffers::FlatBufferBuilder &  _fbb,
const tt::target::Version *  version = nullptr,
const char *  ttmlir_git_hash = nullptr,
::flatbuffers::Offset< tt::target::SystemDesc >  system_desc = 0,
const std::vector<::flatbuffers::Offset< tt::target::metal::Program >> *  programs = nullptr 
)

◆ EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer16 >()

template<>
const tt::target::metal::ConstantBuffer16* tt::target::metal::EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer16 > ( ) const
inline

◆ EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer32 >()

template<>
const tt::target::metal::ConstantBuffer32* tt::target::metal::EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer32 > ( ) const
inline

◆ EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer8 >()

template<>
const tt::target::metal::ConstantBuffer8* tt::target::metal::EnqueueWriteBufferCommand::src_as< tt::target::metal::ConstantBuffer8 > ( ) const
inline

◆ EnqueueWriteBufferCommand::src_as< tt::target::metal::TensorRef >()

template<>
const tt::target::metal::TensorRef* tt::target::metal::EnqueueWriteBufferCommand::src_as< tt::target::metal::TensorRef > ( ) const
inline

◆ EnumNameBinaryType()

const char* tt::target::metal::EnumNameBinaryType ( BinaryType  e)
inline

◆ EnumNameCommandType()

const char* tt::target::metal::EnumNameCommandType ( CommandType  e)
inline

◆ EnumNameCoreType()

const char* tt::target::metal::EnumNameCoreType ( CoreType  e)
inline

◆ EnumNameEthType()

const char* tt::target::metal::EnumNameEthType ( EthType  e)
inline

◆ EnumNameHostBuffer()

const char* tt::target::metal::EnumNameHostBuffer ( HostBuffer  e)
inline

◆ EnumNameKernel()

const char* tt::target::metal::EnumNameKernel ( Kernel  e)
inline

◆ EnumNameKernelConfig()

const char* tt::target::metal::EnumNameKernelConfig ( KernelConfig  e)
inline

◆ EnumNameNocIndex()

const char* tt::target::metal::EnumNameNocIndex ( NocIndex  e)
inline

◆ EnumNameRuntimeArg()

const char* tt::target::metal::EnumNameRuntimeArg ( RuntimeArg  e)
inline

◆ EnumNamesBinaryType()

const char* const* tt::target::metal::EnumNamesBinaryType ( )
inline

◆ EnumNamesCommandType()

const char* const* tt::target::metal::EnumNamesCommandType ( )
inline

◆ EnumNamesCoreType()

const char* const* tt::target::metal::EnumNamesCoreType ( )
inline

◆ EnumNamesEthType()

const char* const* tt::target::metal::EnumNamesEthType ( )
inline

◆ EnumNamesHostBuffer()

const char* const* tt::target::metal::EnumNamesHostBuffer ( )
inline

◆ EnumNamesKernel()

const char* const* tt::target::metal::EnumNamesKernel ( )
inline

◆ EnumNamesKernelConfig()

const char* const* tt::target::metal::EnumNamesKernelConfig ( )
inline

◆ EnumNamesNocIndex()

const char* const* tt::target::metal::EnumNamesNocIndex ( )
inline

◆ EnumNamesRuntimeArg()

const char* const* tt::target::metal::EnumNamesRuntimeArg ( )
inline

◆ EnumNamesUnpackToDestMode()

const char* const* tt::target::metal::EnumNamesUnpackToDestMode ( )
inline

◆ EnumNameUnpackToDestMode()

const char* tt::target::metal::EnumNameUnpackToDestMode ( UnpackToDestMode  e)
inline

◆ EnumValuesBinaryType()

const BinaryType(& tt::target::metal::EnumValuesBinaryType ( ) )[6]
inline

◆ EnumValuesCommandType()

const CommandType(& tt::target::metal::EnumValuesCommandType ( ) )[12]
inline

◆ EnumValuesCoreType()

const CoreType(& tt::target::metal::EnumValuesCoreType ( ) )[2]
inline

◆ EnumValuesEthType()

const EthType(& tt::target::metal::EnumValuesEthType ( ) )[2]
inline

◆ EnumValuesHostBuffer()

const HostBuffer(& tt::target::metal::EnumValuesHostBuffer ( ) )[5]
inline

◆ EnumValuesKernel()

const Kernel(& tt::target::metal::EnumValuesKernel ( ) )[3]
inline

◆ EnumValuesKernelConfig()

const KernelConfig(& tt::target::metal::EnumValuesKernelConfig ( ) )[4]
inline

◆ EnumValuesNocIndex()

const NocIndex(& tt::target::metal::EnumValuesNocIndex ( ) )[2]
inline

◆ EnumValuesRuntimeArg()

const RuntimeArg(& tt::target::metal::EnumValuesRuntimeArg ( ) )[3]
inline

◆ EnumValuesUnpackToDestMode()

const UnpackToDestMode(& tt::target::metal::EnumValuesUnpackToDestMode ( ) )[2]
inline

◆ FinishSizePrefixedTTMetalBinaryBuffer()

void tt::target::metal::FinishSizePrefixedTTMetalBinaryBuffer ( ::flatbuffers::FlatBufferBuilder &  fbb,
::flatbuffers::Offset< tt::target::metal::TTMetalBinary >  root 
)
inline

◆ FinishTTMetalBinaryBuffer()

void tt::target::metal::FinishTTMetalBinaryBuffer ( ::flatbuffers::FlatBufferBuilder &  fbb,
::flatbuffers::Offset< tt::target::metal::TTMetalBinary >  root 
)
inline

◆ GetSizePrefixedTTMetalBinary()

const tt::target::metal::TTMetalBinary* tt::target::metal::GetSizePrefixedTTMetalBinary ( const void *  buf)
inline

◆ GetTTMetalBinary()

const tt::target::metal::TTMetalBinary* tt::target::metal::GetTTMetalBinary ( const void *  buf)
inline

◆ KernelDesc::kernel_as< tt::target::metal::KernelBinary >()

template<>
const tt::target::metal::KernelBinary* tt::target::metal::KernelDesc::kernel_as< tt::target::metal::KernelBinary > ( ) const
inline

◆ KernelDesc::kernel_as< tt::target::metal::KernelSource >()

template<>
const tt::target::metal::KernelSource* tt::target::metal::KernelDesc::kernel_as< tt::target::metal::KernelSource > ( ) const
inline

◆ KernelSource::config_as< tt::target::metal::EthernetConfig >()

template<>
const tt::target::metal::EthernetConfig* tt::target::metal::KernelSource::config_as< tt::target::metal::EthernetConfig > ( ) const
inline

◆ KernelSource::config_as< tt::target::metal::NocConfig >()

template<>
const tt::target::metal::NocConfig* tt::target::metal::KernelSource::config_as< tt::target::metal::NocConfig > ( ) const
inline

◆ KernelSource::config_as< tt::target::metal::TensixConfig >()

template<>
const tt::target::metal::TensixConfig* tt::target::metal::KernelSource::config_as< tt::target::metal::TensixConfig > ( ) const
inline

◆ SizePrefixedTTMetalBinaryBufferHasIdentifier()

bool tt::target::metal::SizePrefixedTTMetalBinaryBufferHasIdentifier ( const void *  buf)
inline

◆ TTMetalBinaryBufferHasIdentifier()

bool tt::target::metal::TTMetalBinaryBufferHasIdentifier ( const void *  buf)
inline

◆ TTMetalBinaryExtension()

const char* tt::target::metal::TTMetalBinaryExtension ( )
inline

◆ TTMetalBinaryIdentifier()

const char* tt::target::metal::TTMetalBinaryIdentifier ( )
inline

◆ VerifyCommandType()

bool tt::target::metal::VerifyCommandType ( ::flatbuffers::Verifier &  verifier,
const void *  obj,
CommandType  type 
)
inline

◆ VerifyCommandTypeVector()

bool tt::target::metal::VerifyCommandTypeVector ( ::flatbuffers::Verifier &  verifier,
const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *  values,
const ::flatbuffers::Vector< CommandType > *  types 
)
inline

◆ VerifyHostBuffer()

bool tt::target::metal::VerifyHostBuffer ( ::flatbuffers::Verifier &  verifier,
const void *  obj,
HostBuffer  type 
)
inline

◆ VerifyHostBufferVector()

bool tt::target::metal::VerifyHostBufferVector ( ::flatbuffers::Verifier &  verifier,
const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *  values,
const ::flatbuffers::Vector< HostBuffer > *  types 
)
inline

◆ VerifyKernel()

bool tt::target::metal::VerifyKernel ( ::flatbuffers::Verifier &  verifier,
const void *  obj,
Kernel  type 
)
inline

◆ VerifyKernelConfig()

bool tt::target::metal::VerifyKernelConfig ( ::flatbuffers::Verifier &  verifier,
const void *  obj,
KernelConfig  type 
)
inline

◆ VerifyKernelConfigVector()

bool tt::target::metal::VerifyKernelConfigVector ( ::flatbuffers::Verifier &  verifier,
const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *  values,
const ::flatbuffers::Vector< KernelConfig > *  types 
)
inline

◆ VerifyKernelVector()

bool tt::target::metal::VerifyKernelVector ( ::flatbuffers::Verifier &  verifier,
const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *  values,
const ::flatbuffers::Vector< Kernel > *  types 
)
inline

◆ VerifyRuntimeArg()

bool tt::target::metal::VerifyRuntimeArg ( ::flatbuffers::Verifier &  verifier,
const void *  obj,
RuntimeArg  type 
)
inline

◆ VerifyRuntimeArgVector()

bool tt::target::metal::VerifyRuntimeArgVector ( ::flatbuffers::Verifier &  verifier,
const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *  values,
const ::flatbuffers::Vector< RuntimeArg > *  types 
)
inline

◆ VerifySizePrefixedTTMetalBinaryBuffer()

bool tt::target::metal::VerifySizePrefixedTTMetalBinaryBuffer ( ::flatbuffers::Verifier &  verifier)
inline

◆ VerifyTTMetalBinaryBuffer()

bool tt::target::metal::VerifyTTMetalBinaryBuffer ( ::flatbuffers::Verifier &  verifier)
inline
Generated by doxygen 1.9.1