DPC++ Runtime
Runtime libraries for oneAPI DPC++
Classes | Typedefs | Enumerations | Functions | Variables
sycl::_V1::detail::pi Namespace Reference

Classes

struct  IsStdVector
 
struct  IsStdVector< std::vector< T > >
 
struct  PiFuncInfo
 
struct  printOut
 
struct  printOut< PiEvent * >
 
struct  printOut< PiMem * >
 
struct  printOut< T ** >
 
struct  printOut< void * >
 

Typedefs

using PiPlugin = ::pi_plugin
 
using PiResult = ::pi_result
 
using PiPlatform = ::pi_platform
 
using PiPlatformBackend = ::pi_platform_backend
 
using PiDevice = ::pi_device
 
using PiDeviceType = ::pi_device_type
 
using PiDeviceInfo = ::pi_device_info
 
using PiDeviceBinaryType = ::pi_device_binary_type
 
using PiContext = ::pi_context
 
using PiContextInfo = ::pi_context_info
 
using PiProgram = ::pi_program
 
using PiKernel = ::pi_kernel
 
using PiQueue = ::pi_queue
 
using PiQueueProperties = ::pi_queue_properties
 
using PiMem = ::pi_mem
 
using PiMemFlags = ::pi_mem_flags
 
using PiEvent = ::pi_event
 
using PiSampler = ::pi_sampler
 
using PiSamplerInfo = ::pi_sampler_info
 
using PiSamplerProperties = ::pi_sampler_properties
 
using PiSamplerAddressingMode = ::pi_sampler_addressing_mode
 
using PiSamplerFilterMode = ::pi_sampler_filter_mode
 
using PiMemImageFormat = ::pi_image_format
 
using PiMemImageDesc = ::pi_image_desc
 
using PiMemImageInfo = ::pi_image_info
 
using PiMemObjectType = ::pi_mem_type
 
using PiMemImageChannelOrder = ::pi_image_channel_order
 
using PiMemImageChannelType = ::pi_image_channel_type
 
using PiKernelCacheConfig = ::pi_kernel_cache_config
 

Enumerations

enum  TraceLevel { PI_TRACE_BASIC = 0x1, PI_TRACE_CALLS = 0x2, PI_TRACE_ALL = -1 }
 

Functions

template<class To >
To cast (std::vector< cl_event > value)
 
template<>
PiDevice cast (cl_device_id)=delete
 
bool trace (TraceLevel level)
 
void die (const char *Message)
 
void assertion (bool Condition, const char *Message=nullptr)
 
template<typename T >
void handleUnknownParamName (const char *functionName, T parameter)
 
void contextSetExtendedDeleter (const sycl::context &constext, pi_context_extended_deleter func, void *user_data)
 
void * loadOsPluginLibrary (const std::string &Library)
 
int unloadOsPluginLibrary (void *Library)
 
int unloadPlugin (void *Library)
 
void * getOsLibraryFuncAddress (void *Library, const std::string &FunctionName)
 
std::string platformInfoToString (pi_platform_info info)
 
template<class To , class From >
To cast (From value)
 
std::vector< PluginPtr > & initialize ()
 
template<backend BE>
const PluginPtr & getPlugin ()
 
uint64_t emitFunctionBeginTrace (const char *FName)
 Emits an XPTI trace before a PI API call is made. More...
 
void emitFunctionEndTrace (uint64_t CorrelationID, const char *FName)
 Emits an XPTI trace after the PI API call has been made. More...
 
uint64_t emitFunctionWithArgsBeginTrace (uint32_t FuncID, const char *FName, unsigned char *ArgsData, pi_plugin Plugin)
 Notifies XPTI subscribers about PI function calls and packs call arguments. More...
 
void emitFunctionWithArgsEndTrace (uint64_t CorrelationID, uint32_t FuncID, const char *FName, unsigned char *ArgsData, pi_result Result, pi_plugin Plugin)
 Notifies XPTI subscribers about PI function call result. More...
 
PiDeviceBinaryType getBinaryImageFormat (const unsigned char *ImgData, size_t ImgSize)
 Tries to determine the device binary image foramat. More...
 
template<class To , class FromE >
To cast (std::vector< FromE > Values)
 
static void initializePlugins (std::vector< PluginPtr > &Plugins)
 
std::string memFlagToString (pi_mem_flags Flag)
 
std::string memFlagsToString (pi_mem_flags Flags)
 
std::vector< std::pair< std::string, backend > > findPlugins ()
 
void * loadPlugin (const std::string &PluginPath)
 
bool bindPlugin (void *Library, const std::shared_ptr< PiPlugin > &PluginInformation)
 
const template PluginPtr & getPlugin< backend::opencl > ()
 
const template PluginPtr & getPlugin< backend::ext_oneapi_level_zero > ()
 
const template PluginPtr & getPlugin< backend::ext_intel_esimd_emulator > ()
 
const template PluginPtr & getPlugin< backend::ext_oneapi_cuda > ()
 
template<typename ResT >
static ResT readELFValue (const unsigned char *Data, size_t NumBytes, bool IsBigEndian)
 
static bool checkELFSectionPresent (const std::string &ExpectedSectionName, const unsigned char *ImgData, size_t ImgSize)
 
static uint16_t getELFHeaderType (const unsigned char *ImgData, size_t ImgSize)
 
template<typename T >
std::enable_if<!std::is_pointer< T >::value, void >::type print (T val)
 
template<typename T >
std::enable_if< std::is_pointer< T >::value, void >::type print (T val)
 
template<>
void print (PiPlatform val)
 
template<>
void print (PiEvent val)
 
template<>
void print (PiMem val)
 
template<>
void print (PiEvent *val)
 
template<>
void print (const PiEvent *val)
 
template<>
void print (pi_buffer_region rgn)
 
template<>
void print (pi_buff_rect_region rgn)
 
template<>
void print (pi_buff_rect_offset off)
 
template<>
void print (pi_image_region rgn)
 
template<>
void print (pi_image_offset off)
 
template<>
void print (const pi_image_desc *desc)
 
template<>
void print (PiResult val)
 
template<>
void print (std::nullptr_t)
 
template<>
void print (char *val)
 
template<>
void print (const char *val)
 
void printArgs (void)
 
template<typename Arg0 , typename... Args>
void printArgs (Arg0 arg0, Args... args)
 
void printOuts (void)
 
template<typename Arg0 , typename... Args>
void printOuts (Arg0 arg0, Args... args)
 
void cuPrint (const char *Message)
 
void hipPrint (const char *Message)
 

Variables

template<>
PiProgram cast (cl_program)=delete
 
std::shared_ptr< plugin > GlobalPlugin
 
bool XPTIInitDone = false
 

Typedef Documentation

◆ PiContext

using sycl::_V1::detail::pi::PiContext = typedef ::pi_context

Definition at line 130 of file pi.hpp.

◆ PiContextInfo

using sycl::_V1::detail::pi::PiContextInfo = typedef ::pi_context_info

Definition at line 131 of file pi.hpp.

◆ PiDevice

using sycl::_V1::detail::pi::PiDevice = typedef ::pi_device

Definition at line 126 of file pi.hpp.

◆ PiDeviceBinaryType

using sycl::_V1::detail::pi::PiDeviceBinaryType = typedef ::pi_device_binary_type

Definition at line 129 of file pi.hpp.

◆ PiDeviceInfo

using sycl::_V1::detail::pi::PiDeviceInfo = typedef ::pi_device_info

Definition at line 128 of file pi.hpp.

◆ PiDeviceType

using sycl::_V1::detail::pi::PiDeviceType = typedef ::pi_device_type

Definition at line 127 of file pi.hpp.

◆ PiEvent

using sycl::_V1::detail::pi::PiEvent = typedef ::pi_event

Definition at line 138 of file pi.hpp.

◆ PiKernel

using sycl::_V1::detail::pi::PiKernel = typedef ::pi_kernel

Definition at line 133 of file pi.hpp.

◆ PiKernelCacheConfig

using sycl::_V1::detail::pi::PiKernelCacheConfig = typedef ::pi_kernel_cache_config

Definition at line 150 of file pi.hpp.

◆ PiMem

using sycl::_V1::detail::pi::PiMem = typedef ::pi_mem

Definition at line 136 of file pi.hpp.

◆ PiMemFlags

using sycl::_V1::detail::pi::PiMemFlags = typedef ::pi_mem_flags

Definition at line 137 of file pi.hpp.

◆ PiMemImageChannelOrder

using sycl::_V1::detail::pi::PiMemImageChannelOrder = typedef ::pi_image_channel_order

Definition at line 148 of file pi.hpp.

◆ PiMemImageChannelType

using sycl::_V1::detail::pi::PiMemImageChannelType = typedef ::pi_image_channel_type

Definition at line 149 of file pi.hpp.

◆ PiMemImageDesc

using sycl::_V1::detail::pi::PiMemImageDesc = typedef ::pi_image_desc

Definition at line 145 of file pi.hpp.

◆ PiMemImageFormat

using sycl::_V1::detail::pi::PiMemImageFormat = typedef ::pi_image_format

Definition at line 144 of file pi.hpp.

◆ PiMemImageInfo

using sycl::_V1::detail::pi::PiMemImageInfo = typedef ::pi_image_info

Definition at line 146 of file pi.hpp.

◆ PiMemObjectType

using sycl::_V1::detail::pi::PiMemObjectType = typedef ::pi_mem_type

Definition at line 147 of file pi.hpp.

◆ PiPlatform

using sycl::_V1::detail::pi::PiPlatform = typedef ::pi_platform

Definition at line 124 of file pi.hpp.

◆ PiPlatformBackend

using sycl::_V1::detail::pi::PiPlatformBackend = typedef ::pi_platform_backend

Definition at line 125 of file pi.hpp.

◆ PiPlugin

using sycl::_V1::detail::pi::PiPlugin = typedef ::pi_plugin

Definition at line 122 of file pi.hpp.

◆ PiProgram

using sycl::_V1::detail::pi::PiProgram = typedef ::pi_program

Definition at line 132 of file pi.hpp.

◆ PiQueue

using sycl::_V1::detail::pi::PiQueue = typedef ::pi_queue

Definition at line 134 of file pi.hpp.

◆ PiQueueProperties

using sycl::_V1::detail::pi::PiQueueProperties = typedef ::pi_queue_properties

Definition at line 135 of file pi.hpp.

◆ PiResult

using sycl::_V1::detail::pi::PiResult = typedef ::pi_result

Definition at line 123 of file pi.hpp.

◆ PiSampler

using sycl::_V1::detail::pi::PiSampler = typedef ::pi_sampler

Definition at line 139 of file pi.hpp.

◆ PiSamplerAddressingMode

using sycl::_V1::detail::pi::PiSamplerAddressingMode = typedef ::pi_sampler_addressing_mode

Definition at line 142 of file pi.hpp.

◆ PiSamplerFilterMode

using sycl::_V1::detail::pi::PiSamplerFilterMode = typedef ::pi_sampler_filter_mode

Definition at line 143 of file pi.hpp.

◆ PiSamplerInfo

using sycl::_V1::detail::pi::PiSamplerInfo = typedef ::pi_sampler_info

Definition at line 140 of file pi.hpp.

◆ PiSamplerProperties

using sycl::_V1::detail::pi::PiSamplerProperties = typedef ::pi_sampler_properties

Definition at line 141 of file pi.hpp.

Enumeration Type Documentation

◆ TraceLevel

enum sycl::_V1::detail::pi::TraceLevel
Enumerator
PI_TRACE_BASIC 
PI_TRACE_CALLS 
PI_TRACE_ALL 

Definition at line 56 of file pi.hpp.

Function Documentation

◆ assertion()

void sycl::_V1::detail::pi::assertion ( bool  Condition,
const char *  Message = nullptr 
)

Definition at line 536 of file pi.cpp.

References die().

Referenced by cast(), cuda_piDeviceGetInfo(), cuda_piEventRelease(), cuda_piEventRetain(), cuda_piKernelGetGroupInfo(), cuda_piKernelGetSubGroupInfo(), cuda_piSamplerRelease(), hip_piDeviceGetInfo(), hip_piEventRelease(), hip_piEventRetain(), hip_piKernelGetGroupInfo(), hip_piKernelGetSubGroupInfo(), hip_piSamplerRelease(), and memFlagToString().

◆ bindPlugin()

bool sycl::_V1::detail::pi::bindPlugin ( void *  Library,
const std::shared_ptr< PiPlugin > &  PluginInformation 
)

Definition at line 370 of file pi.cpp.

References getOsLibraryFuncAddress(), and piPluginInit().

Referenced by initializePlugins().

◆ cast() [1/4]

template<>
PiDevice sycl::_V1::detail::pi::cast ( cl_device_id  )
inlinedelete

◆ cast() [2/4]

template<class To , class From >
To sycl::_V1::detail::pi::cast ( From  value)
inline

Definition at line 254 of file pi.hpp.

References assertion().

◆ cast() [3/4]

template<class To >
To sycl::_V1::detail::pi::cast ( std::vector< cl_event >  value)
inline

Definition at line 164 of file backend_traits_opencl.hpp.

References assertion().

◆ cast() [4/4]

template<class To , class FromE >
To sycl::_V1::detail::pi::cast ( std::vector< FromE >  Values)

Definition at line 266 of file pi.hpp.

◆ checkELFSectionPresent()

static bool sycl::_V1::detail::pi::checkELFSectionPresent ( const std::string &  ExpectedSectionName,
const unsigned char *  ImgData,
size_t  ImgSize 
)
static

Definition at line 558 of file pi.cpp.

Referenced by getBinaryImageFormat().

◆ contextSetExtendedDeleter()

void sycl::_V1::detail::pi::contextSetExtendedDeleter ( const sycl::context &  constext,
pi_context_extended_deleter  func,
void *  user_data 
)

Definition at line 172 of file pi.cpp.

References sycl::_V1::detail::getSyclObjImpl(), and piextContextSetExtendedDeleter().

◆ cuPrint()

void sycl::_V1::detail::pi::cuPrint ( const char *  Message)

Definition at line 467 of file pi_cuda.cpp.

References std::cerr.

Referenced by cuda_piclProgramCreateWithSource(), and cuda_piDeviceGetInfo().

◆ die()

void sycl::_V1::detail::pi::die ( const char *  Message)

Definition at line 531 of file pi.cpp.

References std::cerr.

Referenced by assertion(), cuda_piDeviceGetInfo(), cuda_piEnqueueMemImageFill(), cuda_piEnqueueNativeKernel(), cuda_piEventCreate(), cuda_piEventGetProfilingInfo(), cuda_piEventSetCallback(), cuda_piEventSetStatus(), cuda_piextDeviceSelectBinary(), cuda_piextEnqueueReadHostPipe(), cuda_piextEnqueueWriteHostPipe(), cuda_piextKernelCreateWithNativeHandle(), cuda_piextMemCreateWithNativeHandle(), cuda_piextMemImageCreateWithNativeHandle(), cuda_piextProgramCreateWithNativeHandle(), cuda_piextProgramSetSpecializationConstant(), cuda_piextQueueCreateWithNativeHandle(), cuda_piextUSMEnqueueFill2D(), cuda_piextUSMEnqueueMemAdvise(), cuda_piextUSMEnqueueMemset2D(), cuda_piMemGetInfo(), cuda_piMemImageCreate(), cuda_piMemImageGetInfo(), cuda_piMemRelease(), cuda_piPlatformGetInfo(), cuda_piProgramCreate(), cuda_piProgramGetBuildInfo(), cuda_piProgramGetInfo(), cuda_piQueueGetInfo(), ur_context_handle_t_::decrementUnreleasedEventsInPool(), DieUnsupported(), ur_queue_handle_t_::executeCommandList(), _ur_buffer::free(), getKernelNames(), ur_event_handle_t_::getOrCreateHostVisibleEvent(), _ur_buffer::getZeHandle(), ur_queue_handle_t_::pi_queue_group_t::getZeQueue(), handleUnknownParamName(), hip_piContextCreate(), hip_piDeviceGetInfo(), hip_piEnqueueMemImageFill(), hip_piEnqueueNativeKernel(), hip_piEventCreate(), hip_piEventGetProfilingInfo(), hip_piEventSetCallback(), hip_piEventSetStatus(), hip_piextContextCreateWithNativeHandle(), hip_piextDeviceCreateWithNativeHandle(), hip_piextDeviceSelectBinary(), hip_piextEnqueueDeviceGlobalVariableRead(), hip_piextEnqueueDeviceGlobalVariableWrite(), hip_piextEnqueueReadHostPipe(), hip_piextEnqueueWriteHostPipe(), hip_piextEventCreateWithNativeHandle(), hip_piextKernelSetArgMemObj(), hip_piextMemCreateWithNativeHandle(), hip_piextMemImageCreateWithNativeHandle(), hip_piextProgramCreateWithNativeHandle(), hip_piextProgramSetSpecializationConstant(), hip_piextQueueCreateWithNativeHandle(), hip_piextUSMEnqueueFill2D(), hip_piextUSMEnqueueMemset2D(), hip_piKernelGetGroupInfo(), hip_piMemGetInfo(), hip_piMemImageCreate(), hip_piMemImageGetInfo(), hip_piMemRelease(), hip_piPlatformGetInfo(), hip_piProgramCreate(), hip_piProgramGetBuildInfo(), hip_piProgramGetInfo(), hip_piProgramLink(), hip_piQueueGetInfo(), imageElementByteSize(), pi2ur::pi2urImageDesc(), pi2ur::piclProgramCreateWithSource(), pi2ur::piContextGetInfo(), pi2ur::piEnqueueMemImageFill(), pi2ur::piEnqueueNativeKernel(), pi2ur::piEventSetCallback(), pi2ur::piEventSetStatus(), piextEnqueueReadHostPipe(), piextEnqueueWriteHostPipe(), pi2ur::piextUSMEnqueueMemset2D(), pi2ur::piextUSMGetMemAllocInfo(), pi2ur::piKernelGetGroupInfo(), pi2ur::piKernelSetExecInfo(), pi2ur::piMemBufferCreate(), pi2ur::piMemGetInfo(), piPlatformGetInfo(), pi2ur::piPlatformGetInfo(), pi2ur::piProgramBuild(), pi2ur::piProgramCreateWithBinary(), pi2ur::piProgramGetBuildInfo(), pi2ur::piProgramGetInfo(), pi2ur::piProgramLink(), pi2ur::piQueueGetInfo(), platformInfoToString(), _pi_event::record(), ur2piDeviceInfoValue(), ur2piPlatformInfoValue(), ur2piUSMAllocInfoValue(), ur2zeImageDesc(), urContextGetInfo(), urDeviceGetInfo(), urEventWait(), urKernelGetSubGroupInfo(), urMemBufferCreate(), urMemBufferCreateWithNativeHandle(), urMemBufferPartition(), urMemGetInfo(), urMemImageCreate(), urProgramGetInfo(), urQueueGetInfo(), USMFreeHelper(), ZeCommandListBatchConfig(), ZeMemFreeHelper(), and ReleaseGuard< T >::~ReleaseGuard().

◆ emitFunctionBeginTrace()

uint64_t sycl::_V1::detail::pi::emitFunctionBeginTrace ( const char *  FName)

Emits an XPTI trace before a PI API call is made.

Parameters
FNameThe name of the PI API call
Returns
The correlation ID for the API call that is to be used by the emitFunctionEndTrace() call

Definition at line 76 of file pi.cpp.

References sycl::_V1::detail::SYCL_PICALL_STREAM_NAME.

Referenced by sycl::_V1::detail::plugin::call_nocheck().

◆ emitFunctionEndTrace()

void sycl::_V1::detail::pi::emitFunctionEndTrace ( uint64_t  CorrelationID,
const char *  FName 
)

Emits an XPTI trace after the PI API call has been made.

Parameters
CorrelationIDThe correlation ID for the API call generated by the emitFunctionBeginTrace() call.
FNameThe name of the PI API call

Definition at line 120 of file pi.cpp.

References sycl::_V1::detail::SYCL_PICALL_STREAM_NAME.

Referenced by sycl::_V1::detail::plugin::call_nocheck().

◆ emitFunctionWithArgsBeginTrace()

uint64_t sycl::_V1::detail::pi::emitFunctionWithArgsBeginTrace ( uint32_t  FuncID,
const char *  FName,
unsigned char *  ArgsData,
pi_plugin  Plugin 
)

Notifies XPTI subscribers about PI function calls and packs call arguments.

Parameters
FuncIDis the API hash ID from PiApiID type trait.
FNameThe name of the PI API call.
ArgsDatais a pointer to packed function call arguments.
Pluginis the plugin, which is used to make call.

Definition at line 135 of file pi.cpp.

References sycl::_V1::detail::SYCL_PIDEBUGCALL_STREAM_NAME.

Referenced by sycl::_V1::detail::plugin::call_nocheck().

◆ emitFunctionWithArgsEndTrace()

void sycl::_V1::detail::pi::emitFunctionWithArgsEndTrace ( uint64_t  CorrelationID,
uint32_t  FuncID,
const char *  FName,
unsigned char *  ArgsData,
pi_result  Result,
pi_plugin  Plugin 
)

Notifies XPTI subscribers about PI function call result.

Parameters
CorrelationIDThe correlation ID for the API call generated by the emitFunctionWithArgsBeginTrace() call.
FuncIDis the API hash ID from PiApiID type trait.
FNameThe name of the PI API call.
ArgsDatais a pointer to packed function call arguments.
Resultis function call result value.
Pluginis the plugin, which is used to make call.

Definition at line 155 of file pi.cpp.

References sycl::_V1::detail::SYCL_PIDEBUGCALL_STREAM_NAME.

Referenced by sycl::_V1::detail::plugin::call_nocheck().

◆ findPlugins()

std::vector<std::pair<std::string, backend> > sycl::_V1::detail::pi::findPlugins ( )

Definition at line 265 of file pi.cpp.

References sycl::_V1::detail::ods_target_list::backendCompatible(), sycl::_V1::detail::device_filter_list::get(), std::get(), and sycl::_V1::make_error_code().

Referenced by initializePlugins().

◆ getBinaryImageFormat()

RT::PiDeviceBinaryType sycl::_V1::detail::pi::getBinaryImageFormat ( const unsigned char *  ImgData,
size_t  ImgSize 
)

Tries to determine the device binary image foramat.

Returns PI_DEVICE_BINARY_TYPE_NONE if unsuccessful.

Definition at line 630 of file pi.cpp.

References checkELFSectionPresent(), getELFHeaderType(), PI_DEVICE_BINARY_TYPE_LLVMIR_BITCODE, PI_DEVICE_BINARY_TYPE_NATIVE, PI_DEVICE_BINARY_TYPE_NONE, and PI_DEVICE_BINARY_TYPE_SPIRV.

Referenced by sycl::_V1::detail::ProgramManager::createPIProgram(), sycl::_V1::detail::DynRTDeviceBinaryImage::DynRTDeviceBinaryImage(), and sycl::_V1::detail::RTDeviceBinaryImage::init().

◆ getELFHeaderType()

static uint16_t sycl::_V1::detail::pi::getELFHeaderType ( const unsigned char *  ImgData,
size_t  ImgSize 
)
static

Definition at line 622 of file pi.cpp.

Referenced by getBinaryImageFormat().

◆ getOsLibraryFuncAddress()

void * sycl::_V1::detail::pi::getOsLibraryFuncAddress ( void *  Library,
const std::string &  FunctionName 
)

Definition at line 39 of file posix_pi.cpp.

Referenced by bindPlugin(), and sycl::_V1::ext::intel::experimental::detail::compileToSPIRV().

◆ getPlugin()

template<backend BE>
const PluginPtr & sycl::_V1::detail::pi::getPlugin ( )

Definition at line 504 of file pi.cpp.

References initialize().

Referenced by sycl::_V1::detail::buffer_impl::addInteropObject(), sycl::_V1::detail::queue_impl::createQueue(), sycl::_V1::detail::queue_impl::ext_oneapi_empty(), sycl::_V1::detail::kernel_impl::get(), sycl::_V1::detail::queue_impl::get(), sycl::_V1::detail::device_impl::get_device_info_string(), sycl::_V1::detail::platform_impl::get_info(), sycl::_V1::detail::kernel_impl::get_info(), sycl::_V1::detail::platform_impl::getBackendOption(), sycl::_V1::detail::queue_impl::getExclusiveQueueHandleRef(), sycl::_V1::detail::platform_impl::getNative(), sycl::_V1::detail::queue_impl::getNative(), sycl::_V1::detail::platform_impl::has_extension(), sycl::_V1::detail::queue_impl::get_info< info::queue::reference_count >(), sycl::_V1::detail::queue_impl::wait(), sycl::_V1::detail::event_impl::waitInternal(), sycl::_V1::detail::event_impl::~event_impl(), and sycl::_V1::detail::queue_impl::~queue_impl().

◆ getPlugin< backend::ext_intel_esimd_emulator >()

const template PluginPtr& sycl::_V1::detail::pi::getPlugin< backend::ext_intel_esimd_emulator > ( )

◆ getPlugin< backend::ext_oneapi_cuda >()

const template PluginPtr& sycl::_V1::detail::pi::getPlugin< backend::ext_oneapi_cuda > ( )

◆ getPlugin< backend::ext_oneapi_level_zero >()

const template PluginPtr& sycl::_V1::detail::pi::getPlugin< backend::ext_oneapi_level_zero > ( )

◆ getPlugin< backend::opencl >()

const template PluginPtr& sycl::_V1::detail::pi::getPlugin< backend::opencl > ( )

◆ handleUnknownParamName()

template<typename T >
void sycl::_V1::detail::pi::handleUnknownParamName ( const char *  functionName,
T  parameter 
)

Definition at line 107 of file pi.hpp.

References die().

◆ hipPrint()

void sycl::_V1::detail::pi::hipPrint ( const char *  Message)

Definition at line 417 of file pi_hip.cpp.

References std::cerr.

Referenced by hip_piclProgramCreateWithSource().

◆ initialize()

std::vector< PluginPtr > & sycl::_V1::detail::pi::initialize ( )

Definition at line 396 of file pi.cpp.

References initializePlugins().

Referenced by sycl::_V1::detail::platform_impl::get_devices(), sycl::_V1::detail::platform_impl::get_platforms(), and getPlugin().

◆ initializePlugins()

static void sycl::_V1::detail::pi::initializePlugins ( std::vector< PluginPtr > &  Plugins)
static

Definition at line 406 of file pi.cpp.

References _PI_H_VERSION_STRING, bindPlugin(), std::cerr, findPlugins(), GMajVer, GMinVer, GVerStr, loadPlugin(), PI_TRACE_ALL, PI_TRACE_BASIC, sycl::_V1::detail::SYCL_PICALL_STREAM_NAME, sycl::_V1::detail::SYCL_PIDEBUGCALL_STREAM_NAME, sycl::_V1::detail::SYCL_STREAM_NAME, trace(), and XPTIInitDone.

Referenced by initialize().

◆ loadOsPluginLibrary()

void * sycl::_V1::detail::pi::loadOsPluginLibrary ( const std::string &  Library)

Definition at line 19 of file posix_pi.cpp.

References std::cerr, PI_TRACE_ALL, and trace().

Referenced by sycl::_V1::ext::intel::experimental::detail::compileToSPIRV(), and loadPlugin().

◆ loadPlugin()

void* sycl::_V1::detail::pi::loadPlugin ( const std::string &  PluginPath)

Definition at line 356 of file pi.cpp.

References loadOsPluginLibrary().

Referenced by initializePlugins().

◆ memFlagsToString()

std::string sycl::_V1::detail::pi::memFlagsToString ( pi_mem_flags  Flags)

Definition at line 227 of file pi.cpp.

References memFlagToString(), PI_MEM_FLAGS_ACCESS_RW, PI_MEM_FLAGS_HOST_PTR_COPY, and PI_MEM_FLAGS_HOST_PTR_USE.

◆ memFlagToString()

std::string sycl::_V1::detail::pi::memFlagToString ( pi_mem_flags  Flag)

Definition at line 201 of file pi.cpp.

References assertion(), PI_MEM_FLAGS_ACCESS_RW, PI_MEM_FLAGS_HOST_PTR_COPY, and PI_MEM_FLAGS_HOST_PTR_USE.

Referenced by memFlagsToString().

◆ platformInfoToString()

std::string sycl::_V1::detail::pi::platformInfoToString ( pi_platform_info  info)

Definition at line 182 of file pi.cpp.

References die(), PI_EXT_PLATFORM_INFO_BACKEND, PI_PLATFORM_INFO_EXTENSIONS, PI_PLATFORM_INFO_NAME, PI_PLATFORM_INFO_PROFILE, PI_PLATFORM_INFO_VENDOR, and PI_PLATFORM_INFO_VERSION.

◆ print() [1/17]

template<>
void sycl::_V1::detail::pi::print ( char *  val)
inline

Definition at line 114 of file plugin_printers.hpp.

References std::cout.

◆ print() [2/17]

template<>
void sycl::_V1::detail::pi::print ( const char *  val)
inline

Definition at line 118 of file plugin_printers.hpp.

References std::cout.

Referenced by printArgs().

◆ print() [3/17]

template<>
void sycl::_V1::detail::pi::print ( const pi_image_desc *  desc)
inline

Definition at line 91 of file plugin_printers.hpp.

References std::cout, _pi_image_desc::image_array_size, _pi_image_desc::image_depth, _pi_image_desc::image_height, _pi_image_desc::image_row_pitch, _pi_image_desc::image_slice_pitch, _pi_image_desc::image_type, _pi_image_desc::image_width, _pi_image_desc::num_mip_levels, and _pi_image_desc::num_samples.

◆ print() [4/17]

template<>
void sycl::_V1::detail::pi::print ( const PiEvent *  val)
inline

Definition at line 56 of file plugin_printers.hpp.

References std::cout.

◆ print() [5/17]

template<>
void sycl::_V1::detail::pi::print ( pi_buff_rect_offset  off)
inline

Definition at line 76 of file plugin_printers.hpp.

References std::cout, pi_buff_rect_offset_struct::x_bytes, pi_buff_rect_offset_struct::y_scalar, and pi_buff_rect_offset_struct::z_scalar.

◆ print() [6/17]

template<>
void sycl::_V1::detail::pi::print ( pi_buff_rect_region  rgn)
inline

Definition at line 70 of file plugin_printers.hpp.

References std::cout, pi_buff_rect_region_struct::depth_scalar, pi_buff_rect_region_struct::height_scalar, and pi_buff_rect_region_struct::width_bytes.

◆ print() [7/17]

template<>
void sycl::_V1::detail::pi::print ( pi_buffer_region  rgn)
inline

Definition at line 65 of file plugin_printers.hpp.

References std::cout, pi_buffer_region_struct::origin, and pi_buffer_region_struct::size.

◆ print() [8/17]

template<>
void sycl::_V1::detail::pi::print ( pi_image_offset  off)
inline

Definition at line 86 of file plugin_printers.hpp.

References std::cout, pi_image_offset_struct::x, pi_image_offset_struct::y, and pi_image_offset_struct::z.

◆ print() [9/17]

template<>
void sycl::_V1::detail::pi::print ( pi_image_region  rgn)
inline

Definition at line 81 of file plugin_printers.hpp.

References std::cout, pi_image_region_struct::depth, pi_image_region_struct::height, and pi_image_region_struct::width.

◆ print() [10/17]

template<>
void sycl::_V1::detail::pi::print ( PiEvent *  val)
inline

Definition at line 47 of file plugin_printers.hpp.

References std::cout.

◆ print() [11/17]

template<>
void sycl::_V1::detail::pi::print ( PiEvent  val)
inline

Definition at line 39 of file plugin_printers.hpp.

References std::cout.

◆ print() [12/17]

template<>
void sycl::_V1::detail::pi::print ( PiMem  val)
inline

Definition at line 43 of file plugin_printers.hpp.

References std::cout.

◆ print() [13/17]

template<>
void sycl::_V1::detail::pi::print ( PiPlatform  val)
inline

Definition at line 35 of file plugin_printers.hpp.

References std::cout.

◆ print() [14/17]

template<>
void sycl::_V1::detail::pi::print ( PiResult  val)
inline

Definition at line 101 of file plugin_printers.hpp.

References std::cout.

◆ print() [15/17]

template<>
void sycl::_V1::detail::pi::print ( std::nullptr_t  )
inline

Definition at line 110 of file plugin_printers.hpp.

References std::cout.

◆ print() [16/17]

template<typename T >
std::enable_if<!std::is_pointer<T>::value, void>::type sycl::_V1::detail::pi::print ( T  val)
inline

Definition at line 24 of file plugin_printers.hpp.

References std::cout.

Referenced by sycl::_V1::detail::DynRTDeviceBinaryImage::print().

◆ print() [17/17]

template<typename T >
std::enable_if<std::is_pointer<T>::value, void>::type sycl::_V1::detail::pi::print ( T  val)
inline

Definition at line 30 of file plugin_printers.hpp.

References std::cout.

◆ printArgs() [1/2]

template<typename Arg0 , typename... Args>
void sycl::_V1::detail::pi::printArgs ( Arg0  arg0,
Args...  args 
)

Definition at line 124 of file plugin_printers.hpp.

References std::cout, and print().

◆ printArgs() [2/2]

void sycl::_V1::detail::pi::printArgs ( void  )
inline

Definition at line 122 of file plugin_printers.hpp.

Referenced by sycl::_V1::detail::plugin::call_nocheck().

◆ printOuts() [1/2]

template<typename Arg0 , typename... Args>
void sycl::_V1::detail::pi::printOuts ( Arg0  arg0,
Args...  args 
)

Definition at line 173 of file plugin_printers.hpp.

◆ printOuts() [2/2]

void sycl::_V1::detail::pi::printOuts ( void  )
inline

Definition at line 171 of file plugin_printers.hpp.

Referenced by sycl::_V1::detail::plugin::call_nocheck().

◆ readELFValue()

template<typename ResT >
static ResT sycl::_V1::detail::pi::readELFValue ( const unsigned char *  Data,
size_t  NumBytes,
bool  IsBigEndian 
)
static

Definition at line 543 of file pi.cpp.

◆ trace()

bool sycl::_V1::detail::pi::trace ( TraceLevel  level)

Definition at line 390 of file pi.cpp.

References std::get().

Referenced by sycl::_V1::detail::plugin::call_nocheck(), initializePlugins(), sycl::_V1::detail::IsBannedPlatform(), loadOsPluginLibrary(), sycl::_V1::detail::traceDeviceSelection(), and sycl::_V1::traceDeviceSelector().

◆ unloadOsPluginLibrary()

int sycl::_V1::detail::pi::unloadOsPluginLibrary ( void *  Library)

Definition at line 31 of file posix_pi.cpp.

Referenced by unloadPlugin().

◆ unloadPlugin()

int sycl::_V1::detail::pi::unloadPlugin ( void *  Library)

Definition at line 362 of file pi.cpp.

References unloadOsPluginLibrary().

Referenced by sycl::_V1::detail::plugin::unload().

Variable Documentation

◆ cast

template<>
PiDevice sycl::_V1::detail::pi::cast(cl_device_id)=delete ( cl_program  )
inlinedelete

◆ GlobalPlugin

std::shared_ptr< plugin > sycl::_V1::detail::pi::GlobalPlugin

Definition at line 262 of file pi.cpp.

◆ XPTIInitDone

bool sycl::_V1::detail::pi::XPTIInitDone = false

Definition at line 72 of file pi.cpp.

Referenced by initializePlugins().