tt::target::metal Namespace Reference

Classes
struct	TTMetalBinaryBinarySchema
struct	FLATBUFFERS_FINAL_CLASS
struct	MemoryDescBuilder
struct	LayoutDescBuilder
struct	TensorDescBuilder
struct	TensorRefBuilder
struct	DeviceProgramBuilder
struct	ProgramBuilder
struct	TTMetalBinaryBuilder
struct	CommandTypeTraits
struct	CommandTypeTraits< tt::target::metal::HostAllocCommand >
struct	CommandTypeTraits< tt::target::metal::ReturnCommand >
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	HostAllocCommandBuilder
struct	ReturnCommandBuilder
struct	EnqueueProgramCommandBuilder
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	KernelConfigTypeTraits
struct	KernelConfigTypeTraits< tt::target::metal::NocConfig >
struct	KernelConfigTypeTraits< tt::target::metal::ComputeConfig >
struct	KernelConfigTypeTraits< tt::target::metal::EthernetConfig >
struct	KernelTraits
struct	KernelTraits< tt::target::metal::KernelSource >
struct	KernelTraits< tt::target::metal::KernelBinary >
struct	KernelArgTypeTraits
struct	KernelArgTypeTraits< tt::target::metal::KernelArgCBPort >
struct	KernelArgTypeTraits< tt::target::metal::KernelArgBufferAddress >
struct	KernelArgTypeTraits< tt::target::metal::KernelArgSemaphore >
struct	NocConfigBuilder
struct	ComputeConfigBuilder
struct	EthernetConfigBuilder
struct	KernelSourceBuilder
struct	KernelBinaryBuilder
struct	KernelArgCBPortBuilder
struct	KernelArgBufferAddressBuilder
struct	KernelArgSemaphoreBuilder
struct	KernelArgBuilder
struct	KernelArgsBuilder
struct	KernelConfigBuilder
struct	ProgramDescBuilder
struct	ShardSpecBuilder
struct	ShardSpecBufferBuilder
struct	ShardedBufferConfigBuilder
struct	CircularBufferConfigBuilder
struct	BufferDescBuilder
struct	BufferRefBuilder
struct	CBRefBuilder

Enumerations
enum class	CommandType : uint8_t {   NONE = 0 , HostAllocCommand = 1 , ReturnCommand = 2 , EnqueueProgramCommand = 3 ,   EnqueueWriteBufferCommand = 4 , EnqueueReadBufferCommand = 5 , CreateBufferCommand = 6 , DeallocateBufferCommand = 7 ,   CreateEventCommand = 8 , EnqueueRecordEventCommand = 9 , EnqueueWaitForEventCommand = 10 , EventSynchronizeCommand = 11 ,   EventQueryCommand = 12 , FinishCommand = 13 , 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 { Fp32 = 0 , Default = 1 , MIN = Fp32 , MAX = Default }
enum class	KernelConfigType : uint8_t {   NONE = 0 , NocConfig = 1 , ComputeConfig = 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	KernelArgType : uint8_t {   NONE = 0 , KernelArgCBPort = 1 , KernelArgBufferAddress = 2 , KernelArgSemaphore = 3 ,   MIN = NONE , MAX = KernelArgSemaphore }

Functions
inline ::flatbuffers::Offset< MemoryDesc >	CreateMemoryDesc (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::DataType data_type=tt::target::DataType::Float32)
inline ::flatbuffers::Offset< LayoutDesc >	CreateLayoutDesc (::flatbuffers::FlatBufferBuilder &_fbb, ::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<::flatbuffers::Vector< int32_t >> mesh_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, const std::vector< int32_t > *mesh_shape=nullptr, ::flatbuffers::Offset< tt::target::metal::LayoutDesc > layout=0)
inline ::flatbuffers::Offset< TensorRef >	CreateTensorRef (::flatbuffers::FlatBufferBuilder &_fbb, uint64_t size=0, ::flatbuffers::Offset< tt::target::metal::TensorDesc > desc=0)
inline ::flatbuffers::Offset< DeviceProgram >	CreateDeviceProgram (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::BufferRef >>> inputs=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::BufferRef >>> 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::BufferRef >> *inputs=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::BufferRef >> *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 CommandType(&	EnumValuesCommandType ())[14]
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< HostAllocCommand >	CreateHostAllocCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::BufferRef > dst=0)
inline ::flatbuffers::Offset< ReturnCommand >	CreateReturnCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::BufferRef >>> results=0)
inline ::flatbuffers::Offset< ReturnCommand >	CreateReturnCommandDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector<::flatbuffers::Offset< tt::target::metal::BufferRef >> *results=nullptr)
inline ::flatbuffers::Offset< EnqueueProgramCommand >	CreateEnqueueProgramCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::BufferRef >>> buffers=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::CBRef >>> cbs=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::BufferRef >> *buffers=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::CBRef >> *cbs=nullptr, ::flatbuffers::Offset< tt::target::metal::ProgramDesc > program=0)
inline ::flatbuffers::Offset< EnqueueWriteBufferCommand >	CreateEnqueueWriteBufferCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::BufferRef > src=0, ::flatbuffers::Offset< tt::target::metal::BufferRef > dst=0)
inline ::flatbuffers::Offset< EnqueueReadBufferCommand >	CreateEnqueueReadBufferCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::BufferRef > src=0, ::flatbuffers::Offset< tt::target::metal::BufferRef > dst=0)
inline ::flatbuffers::Offset< CreateBufferCommand >	CreateCreateBufferCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::BufferRef > ref=0)
inline ::flatbuffers::Offset< DeallocateBufferCommand >	CreateDeallocateBufferCommand (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::BufferRef > 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::HostAllocCommand *	Command::type_as< tt::target::metal::HostAllocCommand > () const
template<>
const tt::target::metal::ReturnCommand *	Command::type_as< tt::target::metal::ReturnCommand > () const
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, uint32_t queue_id=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, uint32_t queue_id=0, 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 KernelConfigType(&	EnumValuesKernelConfigType ())[4]
const char *const *	EnumNamesKernelConfigType ()
const char *	EnumNameKernelConfigType (KernelConfigType e)
bool	VerifyKernelConfigType (::flatbuffers::Verifier &verifier, const void *obj, KernelConfigType type)
bool	VerifyKernelConfigTypeVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< KernelConfigType > *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 KernelArgType(&	EnumValuesKernelArgType ())[4]
const char *const *	EnumNamesKernelArgType ()
const char *	EnumNameKernelArgType (KernelArgType e)
bool	VerifyKernelArgType (::flatbuffers::Verifier &verifier, const void *obj, KernelArgType type)
bool	VerifyKernelArgTypeVector (::flatbuffers::Verifier &verifier, const ::flatbuffers::Vector<::flatbuffers::Offset< void >> *values, const ::flatbuffers::Vector< KernelArgType > *types)
inline ::flatbuffers::Offset< NocConfig >	CreateNocConfig (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::NocIndex noc_index=tt::target::metal::NocIndex::Noc0)
inline ::flatbuffers::Offset< ComputeConfig >	CreateComputeConfig (::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< ComputeConfig >	CreateComputeConfigDirect (::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)
inline ::flatbuffers::Offset< KernelSource >	CreateKernelSource (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::String > source=0)
inline ::flatbuffers::Offset< KernelSource >	CreateKernelSourceDirect (::flatbuffers::FlatBufferBuilder &_fbb, const char *source=nullptr)
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< KernelArgCBPort >	CreateKernelArgCBPort (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t operand_idx=0)
inline ::flatbuffers::Offset< KernelArgBufferAddress >	CreateKernelArgBufferAddress (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t operand_idx=0)
inline ::flatbuffers::Offset< KernelArgSemaphore >	CreateKernelArgSemaphore (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t initial_value=0, tt::target::metal::CoreType core_type=tt::target::metal::CoreType::WORKER)
template<>
const tt::target::metal::KernelArgCBPort *	KernelArg::arg_as< tt::target::metal::KernelArgCBPort > () const
template<>
const tt::target::metal::KernelArgBufferAddress *	KernelArg::arg_as< tt::target::metal::KernelArgBufferAddress > () const
template<>
const tt::target::metal::KernelArgSemaphore *	KernelArg::arg_as< tt::target::metal::KernelArgSemaphore > () const
inline ::flatbuffers::Offset< KernelArg >	CreateKernelArg (::flatbuffers::FlatBufferBuilder &_fbb, tt::target::metal::KernelArgType arg_type=tt::target::metal::KernelArgType::NONE, ::flatbuffers::Offset< void > arg=0)
inline ::flatbuffers::Offset< KernelArgs >	CreateKernelArgs (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::KernelArg >>> rt_args=0, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::KernelArg >>> ct_args=0)
inline ::flatbuffers::Offset< KernelArgs >	CreateKernelArgsDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector<::flatbuffers::Offset< tt::target::metal::KernelArg >> *rt_args=nullptr, const std::vector<::flatbuffers::Offset< tt::target::metal::KernelArg >> *ct_args=nullptr)
template<>
const tt::target::metal::KernelSource *	KernelConfig::kernel_as< tt::target::metal::KernelSource > () const
template<>
const tt::target::metal::KernelBinary *	KernelConfig::kernel_as< tt::target::metal::KernelBinary > () const
template<>
const tt::target::metal::NocConfig *	KernelConfig::type_as< tt::target::metal::NocConfig > () const
template<>
const tt::target::metal::ComputeConfig *	KernelConfig::type_as< tt::target::metal::ComputeConfig > () const
template<>
const tt::target::metal::EthernetConfig *	KernelConfig::type_as< tt::target::metal::EthernetConfig > () const
inline ::flatbuffers::Offset< KernelConfig >	CreateKernelConfig (::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< tt::target::metal::KernelArgs > args=0, tt::target::metal::KernelConfigType type_type=tt::target::metal::KernelConfigType::NONE, ::flatbuffers::Offset< void > type=0, ::flatbuffers::Offset<::flatbuffers::String > debug_info=0)
inline ::flatbuffers::Offset< KernelConfig >	CreateKernelConfigDirect (::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, ::flatbuffers::Offset< tt::target::metal::KernelArgs > args=0, tt::target::metal::KernelConfigType type_type=tt::target::metal::KernelConfigType::NONE, ::flatbuffers::Offset< void > type=0, const char *debug_info=nullptr)
inline ::flatbuffers::Offset< ProgramDesc >	CreateProgramDesc (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::KernelConfig >>> kernels=0)
inline ::flatbuffers::Offset< ProgramDesc >	CreateProgramDescDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector<::flatbuffers::Offset< tt::target::metal::KernelConfig >> *kernels=nullptr)
inline ::flatbuffers::Offset< ShardSpec >	CreateShardSpec (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector< const tt::target::Dim2dRange * >> core_range_set=0, const tt::target::Dim2d *shard_shape=nullptr)
inline ::flatbuffers::Offset< ShardSpec >	CreateShardSpecDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector< tt::target::Dim2dRange > *core_range_set=nullptr, const tt::target::Dim2d *shard_shape=nullptr)
inline ::flatbuffers::Offset< ShardSpecBuffer >	CreateShardSpecBuffer (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset< tt::target::metal::ShardSpec > shard_spec=0, const tt::target::Dim2d *page_shape=nullptr, const tt::target::Dim2d *tensor_shape_in_pages=nullptr)
inline ::flatbuffers::Offset< ShardedBufferConfig >	CreateShardedBufferConfig (::flatbuffers::FlatBufferBuilder &_fbb, uint64_t size=0, uint64_t page_size=0, ::flatbuffers::Offset< tt::target::metal::ShardSpecBuffer > shard_spec_buffer=0)
inline ::flatbuffers::Offset< CircularBufferConfig >	CreateCircularBufferConfig (::flatbuffers::FlatBufferBuilder &_fbb, ::flatbuffers::Offset<::flatbuffers::Vector< const tt::target::Dim2dRange * >> core_range_set=0, uint64_t total_size=0, uint64_t page_size=0, uint64_t num_buffers=0)
inline ::flatbuffers::Offset< CircularBufferConfig >	CreateCircularBufferConfigDirect (::flatbuffers::FlatBufferBuilder &_fbb, const std::vector< tt::target::Dim2dRange > *core_range_set=nullptr, uint64_t total_size=0, uint64_t page_size=0, uint64_t num_buffers=0)
inline ::flatbuffers::Offset< BufferDesc >	CreateBufferDesc (::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, ::flatbuffers::Offset< tt::target::metal::ShardedBufferConfig > sharded_buffer_config=0, ::flatbuffers::Offset< tt::target::metal::CircularBufferConfig > circular_buffer_config=0)
inline ::flatbuffers::Offset< BufferDesc >	CreateBufferDescDirect (::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, ::flatbuffers::Offset< tt::target::metal::ShardedBufferConfig > sharded_buffer_config=0, ::flatbuffers::Offset< tt::target::metal::CircularBufferConfig > circular_buffer_config=0)
inline ::flatbuffers::Offset< BufferRef >	CreateBufferRef (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t global_id=0, uint64_t address=0, ::flatbuffers::Offset< tt::target::metal::BufferDesc > desc=0)
inline ::flatbuffers::Offset< CBRef >	CreateCBRef (::flatbuffers::FlatBufferBuilder &_fbb, uint32_t port=0, ::flatbuffers::Offset< tt::target::metal::BufferRef > buffer_ref=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
HostAllocCommand
ReturnCommand
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

Kernel

enum tt::target::metal::Kernel : uint8_t

strong

Enumerator
NONE
KernelSource
KernelBinary
MIN
MAX

KernelArgType

enum tt::target::metal::KernelArgType : uint8_t

strong

Enumerator
NONE
KernelArgCBPort
KernelArgBufferAddress
KernelArgSemaphore
MIN
MAX

KernelConfigType

enum tt::target::metal::KernelConfigType : uint8_t

strong

Enumerator
NONE
NocConfig
ComputeConfig
EthernetConfig
MIN
MAX

NocIndex

enum tt::target::metal::NocIndex : uint16_t

strong

Enumerator
Noc0
Noc1
MIN
MAX

UnpackToDestMode

enum tt::target::metal::UnpackToDestMode : uint8_t

strong

Enumerator
Fp32
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

Command::type_as< tt::target::metal::HostAllocCommand >()

template<>

const tt::target::metal::HostAllocCommand* tt::target::metal::Command::type_as< tt::target::metal::HostAllocCommand > ( ) const

inline

Command::type_as< tt::target::metal::ReturnCommand >()

template<>

const tt::target::metal::ReturnCommand* tt::target::metal::Command::type_as< tt::target::metal::ReturnCommand > ( ) const

inline

CreateBufferDesc()

inline ::flatbuffers::Offset<BufferDesc> tt::target::metal::CreateBufferDesc	(	::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,
		::flatbuffers::Offset< tt::target::metal::ShardedBufferConfig >	sharded_buffer_config = 0,
		::flatbuffers::Offset< tt::target::metal::CircularBufferConfig >	circular_buffer_config = 0
	)

CreateBufferDescDirect()

inline ::flatbuffers::Offset<BufferDesc> tt::target::metal::CreateBufferDescDirect	(	::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,
		::flatbuffers::Offset< tt::target::metal::ShardedBufferConfig >	sharded_buffer_config = 0,
		::flatbuffers::Offset< tt::target::metal::CircularBufferConfig >	circular_buffer_config = 0
	)

CreateBufferRef()

inline ::flatbuffers::Offset<BufferRef> tt::target::metal::CreateBufferRef	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		uint32_t	global_id = 0,
		uint64_t	address = 0,
		::flatbuffers::Offset< tt::target::metal::BufferDesc >	desc = 0
	)

CreateCBRef()

inline ::flatbuffers::Offset<CBRef> tt::target::metal::CreateCBRef	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		uint32_t	port = 0,
		::flatbuffers::Offset< tt::target::metal::BufferRef >	buffer_ref = 0
	)

CreateCircularBufferConfig()

inline ::flatbuffers::Offset<CircularBufferConfig> tt::target::metal::CreateCircularBufferConfig	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset<::flatbuffers::Vector< const tt::target::Dim2dRange * >>	core_range_set = 0,
		uint64_t	total_size = 0,
		uint64_t	page_size = 0,
		uint64_t	num_buffers = 0
	)

CreateCircularBufferConfigDirect()

inline ::flatbuffers::Offset<CircularBufferConfig> tt::target::metal::CreateCircularBufferConfigDirect	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		const std::vector< tt::target::Dim2dRange > *	core_range_set = nullptr,
		uint64_t	total_size = 0,
		uint64_t	page_size = 0,
		uint64_t	num_buffers = 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,
		uint32_t	queue_id = 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,
		uint32_t	queue_id = 0,
		const std::vector<::flatbuffers::Offset< tt::target::metal::Command >> *	commands = nullptr
	)

CreateComputeConfig()

inline ::flatbuffers::Offset<ComputeConfig> tt::target::metal::CreateComputeConfig	(	::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
	)

CreateComputeConfigDirect()

inline ::flatbuffers::Offset<ComputeConfig> tt::target::metal::CreateComputeConfigDirect	(	::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
	)

CreateCreateBufferCommand()

inline ::flatbuffers::Offset<CreateBufferCommand> tt::target::metal::CreateCreateBufferCommand	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset< tt::target::metal::BufferRef >	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::BufferRef >	ref = 0
	)

CreateDeviceProgram()

inline ::flatbuffers::Offset<DeviceProgram> tt::target::metal::CreateDeviceProgram	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::BufferRef >>>	inputs = 0,
		::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::BufferRef >>>	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::BufferRef >> *	inputs = nullptr,
		const std::vector<::flatbuffers::Offset< tt::target::metal::BufferRef >> *	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::BufferRef >>>	buffers = 0,
		::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::CBRef >>>	cbs = 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::BufferRef >> *	buffers = nullptr,
		const std::vector<::flatbuffers::Offset< tt::target::metal::CBRef >> *	cbs = 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::BufferRef >	src = 0,
		::flatbuffers::Offset< tt::target::metal::BufferRef >	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,
		::flatbuffers::Offset< tt::target::metal::BufferRef >	src = 0,
		::flatbuffers::Offset< tt::target::metal::BufferRef >	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

)

CreateHostAllocCommand()

inline ::flatbuffers::Offset<HostAllocCommand> tt::target::metal::CreateHostAllocCommand	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset< tt::target::metal::BufferRef >	dst = 0
	)

CreateKernelArg()

inline ::flatbuffers::Offset<KernelArg> tt::target::metal::CreateKernelArg	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		tt::target::metal::KernelArgType	arg_type = tt::target::metal::KernelArgType::NONE,
		::flatbuffers::Offset< void >	arg = 0
	)

CreateKernelArgBufferAddress()

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

CreateKernelArgCBPort()

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

CreateKernelArgs()

inline ::flatbuffers::Offset<KernelArgs> tt::target::metal::CreateKernelArgs	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::KernelArg >>>	rt_args = 0,
		::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::KernelArg >>>	ct_args = 0
	)

CreateKernelArgsDirect()

inline ::flatbuffers::Offset<KernelArgs> tt::target::metal::CreateKernelArgsDirect	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		const std::vector<::flatbuffers::Offset< tt::target::metal::KernelArg >> *	rt_args = nullptr,
		const std::vector<::flatbuffers::Offset< tt::target::metal::KernelArg >> *	ct_args = nullptr
	)

CreateKernelArgSemaphore()

inline ::flatbuffers::Offset<KernelArgSemaphore> tt::target::metal::CreateKernelArgSemaphore	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		uint32_t	initial_value = 0,
		tt::target::metal::CoreType	core_type = tt::target::metal::CoreType::WORKER
	)

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
	)

CreateKernelConfig()

inline ::flatbuffers::Offset<KernelConfig> tt::target::metal::CreateKernelConfig	(	::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< tt::target::metal::KernelArgs >	args = 0,
		tt::target::metal::KernelConfigType	type_type = tt::target::metal::KernelConfigType::NONE,
		::flatbuffers::Offset< void >	type = 0,
		::flatbuffers::Offset<::flatbuffers::String >	debug_info = 0
	)

CreateKernelConfigDirect()

inline ::flatbuffers::Offset<KernelConfig> tt::target::metal::CreateKernelConfigDirect	(	::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,
		::flatbuffers::Offset< tt::target::metal::KernelArgs >	args = 0,
		tt::target::metal::KernelConfigType	type_type = tt::target::metal::KernelConfigType::NONE,
		::flatbuffers::Offset< void >	type = 0,
		const char *	debug_info = nullptr
	)

CreateKernelSource()

inline ::flatbuffers::Offset<KernelSource> tt::target::metal::CreateKernelSource	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset<::flatbuffers::String >	source = 0
	)

CreateKernelSourceDirect()

inline ::flatbuffers::Offset<KernelSource> tt::target::metal::CreateKernelSourceDirect	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		const char *	source = nullptr
	)

CreateLayoutDesc()

inline ::flatbuffers::Offset<LayoutDesc> tt::target::metal::CreateLayoutDesc	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset< tt::target::metal::MemoryDesc >	memory_desc = 0
	)

CreateMemoryDesc()

inline ::flatbuffers::Offset<MemoryDesc> tt::target::metal::CreateMemoryDesc	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		tt::target::DataType	data_type = tt::target::DataType::Float32
	)

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::KernelConfig >>>	kernels = 0
	)

CreateProgramDescDirect()

inline ::flatbuffers::Offset<ProgramDesc> tt::target::metal::CreateProgramDescDirect	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		const std::vector<::flatbuffers::Offset< tt::target::metal::KernelConfig >> *	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
	)

CreateReturnCommand()

inline ::flatbuffers::Offset<ReturnCommand> tt::target::metal::CreateReturnCommand	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset<::flatbuffers::Vector<::flatbuffers::Offset< tt::target::metal::BufferRef >>>	results = 0
	)

CreateReturnCommandDirect()

inline ::flatbuffers::Offset<ReturnCommand> tt::target::metal::CreateReturnCommandDirect	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		const std::vector<::flatbuffers::Offset< tt::target::metal::BufferRef >> *	results = nullptr
	)

CreateShardedBufferConfig()

inline ::flatbuffers::Offset<ShardedBufferConfig> tt::target::metal::CreateShardedBufferConfig	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		uint64_t	size = 0,
		uint64_t	page_size = 0,
		::flatbuffers::Offset< tt::target::metal::ShardSpecBuffer >	shard_spec_buffer = 0
	)

CreateShardSpec()

inline ::flatbuffers::Offset<ShardSpec> tt::target::metal::CreateShardSpec	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset<::flatbuffers::Vector< const tt::target::Dim2dRange * >>	core_range_set = 0,
		const tt::target::Dim2d *	shard_shape = nullptr
	)

CreateShardSpecBuffer()

inline ::flatbuffers::Offset<ShardSpecBuffer> tt::target::metal::CreateShardSpecBuffer	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset< tt::target::metal::ShardSpec >	shard_spec = 0,
		const tt::target::Dim2d *	page_shape = nullptr,
		const tt::target::Dim2d *	tensor_shape_in_pages = nullptr
	)

CreateShardSpecDirect()

inline ::flatbuffers::Offset<ShardSpec> tt::target::metal::CreateShardSpecDirect	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		const std::vector< tt::target::Dim2dRange > *	core_range_set = nullptr,
		const tt::target::Dim2d *	shard_shape = nullptr
	)

CreateTensorDesc()

inline ::flatbuffers::Offset<TensorDesc> tt::target::metal::CreateTensorDesc	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		::flatbuffers::Offset<::flatbuffers::Vector< int32_t >>	shape = 0,
		::flatbuffers::Offset<::flatbuffers::Vector< int32_t >>	mesh_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,
		const std::vector< int32_t > *	mesh_shape = nullptr,
		::flatbuffers::Offset< tt::target::metal::LayoutDesc >	layout = 0
	)

CreateTensorRef()

inline ::flatbuffers::Offset<TensorRef> tt::target::metal::CreateTensorRef	(	::flatbuffers::FlatBufferBuilder &	_fbb,
		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
	)

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

EnumNameKernel()

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

inline

EnumNameKernelArgType()

const char* tt::target::metal::EnumNameKernelArgType ( KernelArgType  e )

inline

EnumNameKernelConfigType()

const char* tt::target::metal::EnumNameKernelConfigType ( KernelConfigType  e )

inline

EnumNameNocIndex()

const char* tt::target::metal::EnumNameNocIndex ( NocIndex  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

EnumNamesKernel()

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

inline

EnumNamesKernelArgType()

const char* const* tt::target::metal::EnumNamesKernelArgType ( )

inline

EnumNamesKernelConfigType()

const char* const* tt::target::metal::EnumNamesKernelConfigType ( )

inline

EnumNamesNocIndex()

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

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 ( ) )[14]

inline

EnumValuesCoreType()

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

inline

EnumValuesEthType()

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

inline

EnumValuesKernel()

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

inline

EnumValuesKernelArgType()

const KernelArgType(& tt::target::metal::EnumValuesKernelArgType ( ) )[4]

inline

EnumValuesKernelConfigType()

const KernelConfigType(& tt::target::metal::EnumValuesKernelConfigType ( ) )[4]

inline

EnumValuesNocIndex()

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

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

KernelArg::arg_as< tt::target::metal::KernelArgBufferAddress >()

template<>

const tt::target::metal::KernelArgBufferAddress* tt::target::metal::KernelArg::arg_as< tt::target::metal::KernelArgBufferAddress > ( ) const

inline

KernelArg::arg_as< tt::target::metal::KernelArgCBPort >()

template<>

const tt::target::metal::KernelArgCBPort* tt::target::metal::KernelArg::arg_as< tt::target::metal::KernelArgCBPort > ( ) const

inline

KernelArg::arg_as< tt::target::metal::KernelArgSemaphore >()

template<>

const tt::target::metal::KernelArgSemaphore* tt::target::metal::KernelArg::arg_as< tt::target::metal::KernelArgSemaphore > ( ) const

inline

KernelConfig::kernel_as< tt::target::metal::KernelBinary >()

template<>

const tt::target::metal::KernelBinary* tt::target::metal::KernelConfig::kernel_as< tt::target::metal::KernelBinary > ( ) const

inline

KernelConfig::kernel_as< tt::target::metal::KernelSource >()

template<>

const tt::target::metal::KernelSource* tt::target::metal::KernelConfig::kernel_as< tt::target::metal::KernelSource > ( ) const

inline

KernelConfig::type_as< tt::target::metal::ComputeConfig >()

template<>

const tt::target::metal::ComputeConfig* tt::target::metal::KernelConfig::type_as< tt::target::metal::ComputeConfig > ( ) const

inline

KernelConfig::type_as< tt::target::metal::EthernetConfig >()

template<>

const tt::target::metal::EthernetConfig* tt::target::metal::KernelConfig::type_as< tt::target::metal::EthernetConfig > ( ) const

inline

KernelConfig::type_as< tt::target::metal::NocConfig >()

template<>

const tt::target::metal::NocConfig* tt::target::metal::KernelConfig::type_as< tt::target::metal::NocConfig > ( ) 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

VerifyKernel()

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

inline

VerifyKernelArgType()

bool tt::target::metal::VerifyKernelArgType ( ::flatbuffers::Verifier &  verifier, const void *  obj, KernelArgType  type  )

inline

VerifyKernelArgTypeVector()

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

inline

VerifyKernelConfigType()

bool tt::target::metal::VerifyKernelConfigType ( ::flatbuffers::Verifier &  verifier, const void *  obj, KernelConfigType  type  )

inline

VerifyKernelConfigTypeVector()

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

inline

VerifyKernelVector()

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

inline

VerifySizePrefixedTTMetalBinaryBuffer()

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

inline

VerifyTTMetalBinaryBuffer()

bool tt::target::metal::VerifyTTMetalBinaryBuffer ( ::flatbuffers::Verifier &  verifier )

inline