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

Classes

struct  IsStdVector
 
struct  IsStdVector< std::vector< T > >
 

Typedefs

using DeviceBinaryType = ::sycl_device_binary_type
 

Enumerations

enum  TraceLevel { TRACE_BASIC = 0x1 , TRACE_CALLS = 0x2 , TRACE_ALL = -1 }
 

Functions

template<class To >
To cast (std::vector< cl_event > value)
 
template<>
ur_program_handle_t cast (cl_program)=delete
 
template<>
ur_device_handle_t cast (cl_device_id)=delete
 
void * loadOsLibrary (const std::string &Library)
 
int unloadOsLibrary (void *Library)
 
void * getOsLibraryFuncAddress (void *Library, const std::string &FunctionName)
 
void * getURLoaderLibrary ()
 
std::vector< PluginPtr > & initializeUr (ur_loader_config_handle_t LoaderConfig=nullptr)
 
template<backend BE>
const PluginPtr & getPlugin ()
 
bool trace (TraceLevel level)
 
template<class To , class From >
To cast (From value)
 
template<class To , class FromE >
To cast (std::vector< FromE > Values)
 
ur_program_metadata_t mapDeviceBinaryPropertyToProgramMetadata (const sycl_device_binary_property &DeviceBinaryProperty)
 
static void initializePlugins (std::vector< PluginPtr > &Plugins, ur_loader_config_handle_t LoaderConfig)
 
template const PluginPtr & getPlugin< backend::opencl > ()
 
template const PluginPtr & getPlugin< backend::ext_oneapi_level_zero > ()
 
template const PluginPtr & getPlugin< backend::ext_oneapi_cuda > ()
 
template const PluginPtr & getPlugin< backend::ext_oneapi_hip > ()
 
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)
 
sycl_device_binary_type getBinaryImageFormat (const unsigned char *ImgData, size_t ImgSize)
 Tries to determine the device binary image foramat. More...
 
static std::filesystem::path getCurrentDSODirPath ()
 

Variables

bool XPTIInitDone = false
 

Typedef Documentation

◆ DeviceBinaryType

using sycl::_V1::detail::ur::DeviceBinaryType = typedef ::sycl_device_binary_type

Definition at line 72 of file ur_utils.hpp.

Enumeration Type Documentation

◆ TraceLevel

enum sycl::_V1::detail::ur::TraceLevel
Enumerator
TRACE_BASIC 
TRACE_CALLS 
TRACE_ALL 

Definition at line 137 of file ur.hpp.

Function Documentation

◆ cast() [1/5]

template<>
ur_device_handle_t sycl::_V1::detail::ur::cast ( cl_device_id  )
inlinedelete

◆ cast() [2/5]

template<>
ur_program_handle_t sycl::_V1::detail::ur::cast ( cl_program  )
inlinedelete

◆ cast() [3/5]

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

Definition at line 147 of file ur.hpp.

◆ cast() [4/5]

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

Definition at line 145 of file backend_traits_opencl.hpp.

Referenced by sycl::_V1::detail::BufferInterop< backend::opencl, DataT, Dimensions, AllocatorT >::GetNativeObjs().

◆ cast() [5/5]

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

Definition at line 159 of file ur.hpp.

◆ checkELFSectionPresent()

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

Definition at line 303 of file ur.cpp.

Referenced by getBinaryImageFormat().

◆ getBinaryImageFormat()

DeviceBinaryType sycl::_V1::detail::ur::getBinaryImageFormat ( const unsigned char *  ImgData,
size_t  ImgSize 
)

Tries to determine the device binary image foramat.

Returns SYCL_DEVICE_BINARY_TYPE_NONE if unsuccessful.

Definition at line 376 of file ur.cpp.

References checkELFSectionPresent(), getELFHeaderType(), SYCL_DEVICE_BINARY_TYPE_LLVMIR_BITCODE, SYCL_DEVICE_BINARY_TYPE_NATIVE, SYCL_DEVICE_BINARY_TYPE_NONE, and SYCL_DEVICE_BINARY_TYPE_SPIRV.

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

◆ getCurrentDSODirPath()

static std::filesystem::path sycl::_V1::detail::ur::getCurrentDSODirPath ( )
static

Definition at line 60 of file windows_ur.cpp.

References ExeModuleHandle, and getOSModuleHandle().

◆ getELFHeaderType()

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

Definition at line 368 of file ur.cpp.

Referenced by getBinaryImageFormat().

◆ getOsLibraryFuncAddress()

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

Definition at line 34 of file posix_ur.cpp.

Referenced by sycl::_V1::ext::__SYCL2020_DEPRECATED(), sycl::_V1::ext::oneapi::experimental::detail::checkOclocLibrary(), and sycl::_V1::ext::oneapi::experimental::detail::SetupLibrary().

◆ getPlugin()

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

Definition at line 266 of file ur.cpp.

References initializeUr(), and sycl::_V1::runtime.

◆ getPlugin< backend::ext_oneapi_cuda >()

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

◆ getPlugin< backend::ext_oneapi_hip >()

template const PluginPtr& sycl::_V1::detail::ur::getPlugin< backend::ext_oneapi_hip > ( )

◆ getPlugin< backend::ext_oneapi_level_zero >()

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

◆ getPlugin< backend::opencl >()

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

◆ getURLoaderLibrary()

void * sycl::_V1::detail::ur::getURLoaderLibrary ( )

Definition at line 38 of file posix_ur.cpp.

Referenced by sycl::_V1::detail::ProgramManager::build(), sycl::_V1::detail::ProgramManager::getBuiltURProgram(), sycl::_V1::detail::ProgramManager::getOrCreateMaterializedKernel(), initializePlugins(), sycl::_V1::detail::plugin::plugin(), and sycl::_V1::detail::GlobalHandler::unloadPlugins().

◆ initializePlugins()

static void sycl::_V1::detail::ur::initializePlugins ( std::vector< PluginPtr > &  Plugins,
ur_loader_config_handle_t  LoaderConfig 
)
static

Definition at line 113 of file ur.cpp.

References sycl::_V1::all, std::cerr, CHECK_UR_SUCCESS, sycl::_V1::detail::codeLocationCallback(), sycl::_V1::ext_oneapi_cuda, sycl::_V1::ext_oneapi_hip, sycl::_V1::ext_oneapi_level_zero, sycl::_V1::ext_oneapi_native_cpu, sycl::_V1::detail::ProgramManager::getInstance(), getURLoaderLibrary(), sycl::_V1::detail::GlobalHandler::getXPTIRegistry(), sycl::_V1::detail::XPTIRegistry::initializeFrameworkOnce(), sycl::_V1::detail::XPTIRegistry::initializeStream(), sycl::_V1::detail::GlobalHandler::instance(), sycl::_V1::opencl, sycl::_V1::detail::SYCL_STREAM_NAME, trace(), TRACE_BASIC, TRACE_CALLS, and XPTIInitDone.

Referenced by initializeUr().

◆ initializeUr()

std::vector< PluginPtr > & sycl::_V1::detail::ur::initializeUr ( ur_loader_config_handle_t  LoaderConfig = nullptr)

Definition at line 92 of file ur.cpp.

References std::cerr, sycl::_V1::detail::GlobalHandler::getPlugins(), initializePlugins(), and sycl::_V1::detail::GlobalHandler::instance().

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

◆ loadOsLibrary()

void * sycl::_V1::detail::ur::loadOsLibrary ( const std::string &  Library)

Definition at line 20 of file posix_ur.cpp.

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

Referenced by sycl::_V1::ext::__SYCL2020_DEPRECATED(), and sycl::_V1::ext::oneapi::experimental::detail::loadOclocLibrary().

◆ mapDeviceBinaryPropertyToProgramMetadata()

ur_program_metadata_t sycl::_V1::detail::ur::mapDeviceBinaryPropertyToProgramMetadata ( const sycl_device_binary_property &  DeviceBinaryProperty)

Definition at line 423 of file ur.cpp.

References SYCL_PROPERTY_TYPE_BYTE_ARRAY, SYCL_PROPERTY_TYPE_STRING, and SYCL_PROPERTY_TYPE_UINT32.

Referenced by sycl::_V1::detail::RTDeviceBinaryImage::init().

◆ readELFValue()

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

Definition at line 288 of file ur.cpp.

References sycl::_V1::ext::oneapi::experimental::copy().

◆ trace()

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

Definition at line 81 of file ur.cpp.

References sycl::_V1::detail::SYCLConfig< Config >::get().

Referenced by initializePlugins(), sycl::_V1::detail::IsBannedPlatform(), loadOsLibrary(), and sycl::_V1::detail::traceDeviceSelection().

◆ unloadOsLibrary()

int sycl::_V1::detail::ur::unloadOsLibrary ( void *  Library)

Definition at line 32 of file posix_ur.cpp.

Variable Documentation

◆ XPTIInitDone

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

Definition at line 89 of file ur.cpp.

Referenced by initializePlugins().