DPC++ Runtime
Runtime libraries for oneAPI DPC++
Classes | Public Member Functions | Protected Member Functions | Protected Attributes | List of all members
sycl::_V1::detail::RTDeviceBinaryImage Class Reference

#include <detail/device_binary_image.hpp>

Inheritance diagram for sycl::_V1::detail::RTDeviceBinaryImage:
Inheritance graph
[legend]
Collaboration diagram for sycl::_V1::detail::RTDeviceBinaryImage:
Collaboration graph
[legend]

Classes

class  PropertyRange
 

Public Member Functions

 RTDeviceBinaryImage (OSModuleHandle ModuleHandle)
 
 RTDeviceBinaryImage (pi_device_binary Bin, OSModuleHandle ModuleHandle)
 
 RTDeviceBinaryImage (const RTDeviceBinaryImage &)=delete
 
RTDeviceBinaryImage & operator= (const RTDeviceBinaryImage &)=delete
 
 RTDeviceBinaryImage (RTDeviceBinaryImage &&)=default
 
RTDeviceBinaryImage & operator= (RTDeviceBinaryImage &&)=default
 
OSModuleHandle getOSModuleHandle () const
 
virtual ~RTDeviceBinaryImage ()
 
bool supportsSpecConstants () const
 
const pi_device_binary_struct & getRawData () const
 
virtual void print () const
 
virtual void dump (std::ostream &Out) const
 
size_t getSize () const
 
const char * getCompileOptions () const
 
const char * getLinkOptions () const
 
pi::PiDeviceBinaryType getFormat () const
 Returns the format of the binary image. More...
 
pi_device_binary_property getProperty (const char *PropName) const
 Returns a single property from SYCL_MISC_PROP category. More...
 
const PropertyRange & getSpecConstants () const
 Gets the iterator range over specialization constants in this binary image. More...
 
const PropertyRange & getSpecConstantsDefaultValues () const
 
const PropertyRange & getDeviceLibReqMask () const
 
const PropertyRange & getKernelParamOptInfo () const
 
const PropertyRange & getAssertUsed () const
 
const PropertyRange & getProgramMetadata () const
 
const PropertyRange & getExportedSymbols () const
 
const PropertyRange & getDeviceGlobals () const
 
const PropertyRange & getDeviceRequirements () const
 
const PropertyRange & getHostPipes () const
 
std::uintptr_t getImageID () const
 

Protected Member Functions

void init (pi_device_binary Bin)
 
pi_device_binary get () const
 

Protected Attributes

pi_device_binary Bin
 
OSModuleHandle ModuleHandle
 
pi::PiDeviceBinaryType Format = PI_DEVICE_BINARY_TYPE_NONE
 
RTDeviceBinaryImage::PropertyRange SpecConstIDMap
 
RTDeviceBinaryImage::PropertyRange SpecConstDefaultValuesMap
 
RTDeviceBinaryImage::PropertyRange DeviceLibReqMask
 
RTDeviceBinaryImage::PropertyRange KernelParamOptInfo
 
RTDeviceBinaryImage::PropertyRange AssertUsed
 
RTDeviceBinaryImage::PropertyRange ProgramMetadata
 
RTDeviceBinaryImage::PropertyRange ExportedSymbols
 
RTDeviceBinaryImage::PropertyRange DeviceGlobals
 
RTDeviceBinaryImage::PropertyRange DeviceRequirements
 
RTDeviceBinaryImage::PropertyRange HostPipes
 

Detailed Description

Definition at line 82 of file device_binary_image.hpp.

Constructor & Destructor Documentation

◆ RTDeviceBinaryImage() [1/4]

sycl::_V1::detail::RTDeviceBinaryImage::RTDeviceBinaryImage ( OSModuleHandle  ModuleHandle)
inline

Definition at line 135 of file device_binary_image.hpp.

◆ RTDeviceBinaryImage() [2/4]

sycl::_V1::detail::RTDeviceBinaryImage::RTDeviceBinaryImage ( pi_device_binary  Bin,
OSModuleHandle  ModuleHandle 
)
inline

Definition at line 137 of file device_binary_image.hpp.

◆ RTDeviceBinaryImage() [3/4]

sycl::_V1::detail::RTDeviceBinaryImage::RTDeviceBinaryImage ( const RTDeviceBinaryImage &  )
delete

◆ RTDeviceBinaryImage() [4/4]

sycl::_V1::detail::RTDeviceBinaryImage::RTDeviceBinaryImage ( RTDeviceBinaryImage &&  )
default

◆ ~RTDeviceBinaryImage()

virtual sycl::_V1::detail::RTDeviceBinaryImage::~RTDeviceBinaryImage ( )
inlinevirtual

Definition at line 151 of file device_binary_image.hpp.

Member Function Documentation

◆ dump()

void sycl::_V1::detail::RTDeviceBinaryImage::dump ( std::ostream &  Out) const
virtual

Definition at line 135 of file device_binary_image.cpp.

References pi_device_binary_struct::BinaryStart.

◆ get()

pi_device_binary sycl::_V1::detail::RTDeviceBinaryImage::get ( ) const
inlineprotected

Definition at line 234 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::ProgramManager::getBuiltPIProgram(), and sycl::_V1::detail::ProgramManager::getDeviceImage().

◆ getAssertUsed()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getAssertUsed ( ) const
inline

Definition at line 218 of file device_binary_image.hpp.

◆ getCompileOptions()

const char* sycl::_V1::detail::RTDeviceBinaryImage::getCompileOptions ( ) const
inline

Definition at line 167 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::appendCompileOptionsFromImage().

◆ getDeviceGlobals()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getDeviceGlobals ( ) const
inline

Definition at line 221 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::appendCompileOptionsFromImage().

◆ getDeviceLibReqMask()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getDeviceLibReqMask ( ) const
inline

Definition at line 214 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::ProgramManager::getDeviceLibReqMask().

◆ getDeviceRequirements()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getDeviceRequirements ( ) const
inline

Definition at line 222 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::doesDevSupportDeviceRequirements(), and sycl::_V1::detail::ProgramManager::getBuiltPIProgram().

◆ getExportedSymbols()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getExportedSymbols ( ) const
inline

Definition at line 220 of file device_binary_image.hpp.

◆ getFormat()

pi::PiDeviceBinaryType sycl::_V1::detail::RTDeviceBinaryImage::getFormat ( ) const
inline

Returns the format of the binary image.

Definition at line 178 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::ProgramManager::createPIProgram(), and sycl::_V1::detail::ProgramManager::getBuiltPIProgram().

◆ getHostPipes()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getHostPipes ( ) const
inline

Definition at line 225 of file device_binary_image.hpp.

◆ getImageID()

std::uintptr_t sycl::_V1::detail::RTDeviceBinaryImage::getImageID ( ) const
inline

Definition at line 227 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::ProgramManager::getBuiltPIProgram(), and sycl::_V1::detail::context_impl::getProgramForHostPipe().

◆ getKernelParamOptInfo()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getKernelParamOptInfo ( ) const
inline

Definition at line 215 of file device_binary_image.hpp.

◆ getLinkOptions()

const char* sycl::_V1::detail::RTDeviceBinaryImage::getLinkOptions ( ) const
inline

Definition at line 172 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::appendLinkOptionsFromImage().

◆ getOSModuleHandle()

OSModuleHandle sycl::_V1::detail::RTDeviceBinaryImage::getOSModuleHandle ( ) const
inline

Definition at line 149 of file device_binary_image.hpp.

◆ getProgramMetadata()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getProgramMetadata ( ) const
inline

Definition at line 219 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::ProgramManager::createPIProgram(), and sycl::_V1::detail::ProgramManager::getOrCreatePIProgram().

◆ getProperty()

pi_device_binary_property sycl::_V1::detail::RTDeviceBinaryImage::getProperty ( const char *  PropName) const

Returns a single property from SYCL_MISC_PROP category.

Definition at line 141 of file device_binary_image.cpp.

References __SYCL_PI_PROPERTY_SET_SYCL_MISC_PROP, sycl::_V1::detail::RTDeviceBinaryImage::PropertyRange::begin(), sycl::_V1::detail::RTDeviceBinaryImage::PropertyRange::end(), and sycl::_V1::detail::RTDeviceBinaryImage::PropertyRange::isAvailable().

Referenced by sycl::_V1::detail::appendCompileOptionsForRegAllocMode(), sycl::_V1::detail::getUint32PropAsBool(), and sycl::_V1::detail::getUint32PropAsOptStr().

◆ getRawData()

const pi_device_binary_struct& sycl::_V1::detail::RTDeviceBinaryImage::getRawData ( ) const
inline

Definition at line 157 of file device_binary_image.hpp.

References std::get().

Referenced by sycl::_V1::detail::compatibleWithDevice(), sycl::_V1::detail::ProgramManager::createPIProgram(), sycl::_V1::detail::ProgramManager::flushSpecConstants(), sycl::_V1::detail::getBinImageState(), sycl::_V1::detail::PersistentDeviceCodeCache::getCacheItemPath(), and sycl::_V1::detail::ProgramManager::getDeviceImage().

◆ getSize()

size_t sycl::_V1::detail::RTDeviceBinaryImage::getSize ( ) const
inline

Definition at line 162 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::ProgramManager::createPIProgram(), and sycl::_V1::detail::PersistentDeviceCodeCache::getCacheItemPath().

◆ getSpecConstants()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getSpecConstants ( ) const
inline

Gets the iterator range over specialization constants in this binary image.

For each property pointed to by an iterator within the range, the name of the property is the specialization constant symbolic ID and the value is a list of 3-element tuples of 32-bit unsigned integers, describing the specialization constant. This is done in order to unify representation of both scalar and composite specialization constants: composite specialization constant is represented by its leaf elements, so for scalars the list contains only a single tuple, while for composite there might be more of them. Each tuple consists of ID of scalar specialization constant, its location within a composite (offset in bytes from the beginning or 0 if it is not an element of a composite specialization constant) and its size. For example, for the following structure: struct A { int a; float b; }; struct POD { A a[2]; int b; }; List of tuples will look like: { ID0, 0, 4 }, // .a[0].a { ID1, 4, 4 }, // .a[0].b { ID2, 8, 4 }, // .a[1].a { ID3, 12, 4 }, // .a[1].b { ID4, 16, 4 }, // .b And for an interger specialization constant, the list of tuples will look like: { ID5, 0, 4 }

Definition at line 210 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::program_impl::flush_spec_constants().

◆ getSpecConstantsDefaultValues()

const PropertyRange& sycl::_V1::detail::RTDeviceBinaryImage::getSpecConstantsDefaultValues ( ) const
inline

Definition at line 211 of file device_binary_image.hpp.

◆ init()

void sycl::_V1::detail::RTDeviceBinaryImage::init ( pi_device_binary  Bin)
protected

Definition at line 156 of file device_binary_image.cpp.

References __SYCL_PI_PROPERTY_SET_DEVICELIB_REQ_MASK, __SYCL_PI_PROPERTY_SET_KERNEL_PARAM_OPT_INFO, __SYCL_PI_PROPERTY_SET_PROGRAM_METADATA, __SYCL_PI_PROPERTY_SET_SPEC_CONST_DEFAULT_VALUES_MAP, __SYCL_PI_PROPERTY_SET_SPEC_CONST_MAP, __SYCL_PI_PROPERTY_SET_SYCL_ASSERT_USED, __SYCL_PI_PROPERTY_SET_SYCL_DEVICE_GLOBALS, __SYCL_PI_PROPERTY_SET_SYCL_DEVICE_REQUIREMENTS, __SYCL_PI_PROPERTY_SET_SYCL_EXPORTED_SYMBOLS, __SYCL_PI_PROPERTY_SET_SYCL_HOST_PIPES, pi_device_binary_struct::BinaryStart, pi_device_binary_struct::Format, sycl::_V1::detail::pi::getBinaryImageFormat(), and PI_DEVICE_BINARY_TYPE_NONE.

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

◆ operator=() [1/2]

RTDeviceBinaryImage& sycl::_V1::detail::RTDeviceBinaryImage::operator= ( const RTDeviceBinaryImage &  )
delete

◆ operator=() [2/2]

RTDeviceBinaryImage& sycl::_V1::detail::RTDeviceBinaryImage::operator= ( RTDeviceBinaryImage &&  )
default

◆ print()

void sycl::_V1::detail::RTDeviceBinaryImage::print ( ) const
virtual

Reimplemented in sycl::_V1::detail::DynRTDeviceBinaryImage.

Definition at line 100 of file device_binary_image.cpp.

References std::cerr, _pi_device_binary_property_set_struct::Name, _pi_device_binary_property_set_struct::PropertiesBegin, and _pi_device_binary_property_set_struct::PropertiesEnd.

Referenced by sycl::_V1::detail::ProgramManager::getDeviceImage().

◆ supportsSpecConstants()

bool sycl::_V1::detail::RTDeviceBinaryImage::supportsSpecConstants ( ) const
inline

Definition at line 153 of file device_binary_image.hpp.

References PI_DEVICE_BINARY_TYPE_SPIRV.

Referenced by sycl::_V1::detail::ProgramManager::flushSpecConstants(), and sycl::_V1::detail::ProgramManager::getBuiltPIProgram().

Member Data Documentation

◆ AssertUsed

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::AssertUsed
protected

Definition at line 244 of file device_binary_image.hpp.

◆ Bin

pi_device_binary sycl::_V1::detail::RTDeviceBinaryImage::Bin
protected

Definition at line 236 of file device_binary_image.hpp.

Referenced by sycl::_V1::detail::DynRTDeviceBinaryImage::DynRTDeviceBinaryImage(), and sycl::_V1::detail::DynRTDeviceBinaryImage::~DynRTDeviceBinaryImage().

◆ DeviceGlobals

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::DeviceGlobals
protected

Definition at line 247 of file device_binary_image.hpp.

◆ DeviceLibReqMask

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::DeviceLibReqMask
protected

Definition at line 242 of file device_binary_image.hpp.

◆ DeviceRequirements

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::DeviceRequirements
protected

Definition at line 248 of file device_binary_image.hpp.

◆ ExportedSymbols

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::ExportedSymbols
protected

Definition at line 246 of file device_binary_image.hpp.

◆ Format

pi::PiDeviceBinaryType sycl::_V1::detail::RTDeviceBinaryImage::Format = PI_DEVICE_BINARY_TYPE_NONE
protected

Definition at line 239 of file device_binary_image.hpp.

◆ HostPipes

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::HostPipes
protected

Definition at line 249 of file device_binary_image.hpp.

◆ KernelParamOptInfo

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::KernelParamOptInfo
protected

Definition at line 243 of file device_binary_image.hpp.

◆ ModuleHandle

OSModuleHandle sycl::_V1::detail::RTDeviceBinaryImage::ModuleHandle
protected

Definition at line 237 of file device_binary_image.hpp.

◆ ProgramMetadata

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::ProgramMetadata
protected

Definition at line 245 of file device_binary_image.hpp.

◆ SpecConstDefaultValuesMap

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::SpecConstDefaultValuesMap
protected

Definition at line 241 of file device_binary_image.hpp.

◆ SpecConstIDMap

RTDeviceBinaryImage::PropertyRange sycl::_V1::detail::RTDeviceBinaryImage::SpecConstIDMap
protected

Definition at line 240 of file device_binary_image.hpp.

The documentation for this class was generated from the following files: