PI context mapping to a CUDA context object. More...

#include <cuda/pi_cuda.hpp>

Inheritance diagram for _pi_context:

Collaboration diagram for _pi_context:

[legend]

Classes
struct	deleter_data

Public Types
enum	kind { kind::primary, kind::user_defined }

using	native_type = CUcontext

using	native_type = hipCtx_t

Public Member Functions
	_pi_context (_pi_device *devId)

	~_pi_context ()

void	invoke_extended_deleters ()

void	set_extended_deleter (pi_context_extended_deleter function, void *user_data)

pi_device	get_device () const noexcept

native_type	get () const noexcept

pi_uint32	increment_reference_count () noexcept

pi_uint32	decrement_reference_count () noexcept

pi_uint32	get_reference_count () const noexcept

	_pi_context (pi_device ArgDevice)

bool	checkSurfaceArgument (pi_mem_flags Flags, void *HostPtr)

	_pi_context (kind k, hipCtx_t ctxt, _pi_device *devId)

	~_pi_context ()

void	invoke_extended_deleters ()

void	set_extended_deleter (pi_context_extended_deleter function, void *user_data)

pi_device	get_device () const noexcept

native_type	get () const noexcept

bool	is_primary () const noexcept

pi_uint32	increment_reference_count () noexcept

pi_uint32	decrement_reference_count () noexcept

pi_uint32	get_reference_count () const noexcept

	_pi_context (ze_context_handle_t ZeContext, pi_uint32 NumDevices, const pi_device *Devs, bool OwnZeContext)

pi_result	initialize ()

pi_result	finalize ()

pi_platform	getPlatform () const

bool	isValidDevice (pi_device Device) const

pi_result	getAvailableCommandList (pi_queue Queue, pi_command_list_ptr_t &CommandList, bool UseCopyEngine, bool AllowBatching=false, ze_command_queue_handle_t *ForcedCmdQueue=nullptr)

pi_result	getFreeSlotInExistingOrNewPool (ze_event_pool_handle_t &, size_t &, bool HostVisible, bool ProfilingEnabled)

pi_result	decrementUnreleasedEventsInPool (pi_event Event)

pi_event	getEventFromContextCache (bool HostVisible, bool WithProfiling)

void	addEventToContextCache (pi_event)

Public Attributes
native_type	cuContext_

_pi_device *	deviceId_

std::atomic_uint32_t	refCount_

pi_device	Device

std::unordered_map< void , cm_support::CmBufferSVM >	Addr2CmBufferSVM

std::mutex	Addr2CmBufferSVMLock

enum _pi_context::kind	kind_

native_type	hipContext_

const ze_context_handle_t	ZeContext

bool	OwnZeContext

const std::vector< pi_device >	Devices

const pi_device	SingleRootDevice = nullptr

ze_command_list_handle_t	ZeCommandListInit

pi_mutex	ImmediateCommandListMutex

pi_mutex	ZeCommandListCacheMutex

std::unordered_map< ze_device_handle_t, std::list< ze_command_list_handle_t > >	ZeComputeCommandListCache

std::unordered_map< ze_device_handle_t, std::list< ze_command_list_handle_t > >	ZeCopyCommandListCache

std::unordered_map< ze_device_handle_t, USMAllocContext >	DeviceMemAllocContexts

std::unordered_map< ze_device_handle_t, USMAllocContext >	SharedMemAllocContexts

std::unordered_map< ze_device_handle_t, USMAllocContext >	SharedReadOnlyMemAllocContexts

std::unordered_set< void * >	SharedReadOnlyAllocs

std::unique_ptr< USMAllocContext >	HostMemAllocContext

std::unordered_map< void *, MemAllocRecord >	MemAllocs

Detailed Description

PI context mapping to a CUDA context object.

PI context mapping to a HIP context object.

There is no direct mapping between a CUDA context and a PI context, main differences described below:

CUDA context vs PI context

One of the main differences between the PI API and the CUDA driver API is that the second modifies the state of the threads by assigning CUcontext objects to threads. CUcontext objects store data associated with a given device and control access to said device from the user side. PI API context are objects that are passed to functions, and not bound to threads. The _pi_context object doesn't implement this behavior, only holds the CUDA context data. The RAII object ScopedContext implements the active context behavior.

Primary vs User-defined context

CUDA has two different types of context, the Primary context, which is usable by all threads on a given process for a given device, and the aforementioned custom contexts. CUDA documentation, and performance analysis, indicates it is recommended to use Primary context whenever possible. Primary context is used as well by the CUDA Runtime API. For PI applications to interop with CUDA Runtime API, they have to use the primary context - and make that active in the thread. The _pi_context object can be constructed with a kind parameter that allows to construct a Primary or user-defined context, so that the PI object interface is always the same.

Destructor callback

Required to implement CP023, SYCL Extended Context Destruction, the PI Context can store a number of callback functions that will be called upon destruction of the PI Context. See proposal for details.

There is no direct mapping between a HIP context and a PI context, main differences described below:

HIP context vs PI context

One of the main differences between the PI API and the HIP driver API is that the second modifies the state of the threads by assigning hipCtx_t objects to threads. hipCtx_t objects store data associated with a given device and control access to said device from the user side. PI API context are objects that are passed to functions, and not bound to threads. The _pi_context object doesn't implement this behavior, only holds the HIP context data. The RAII object ScopedContext implements the active context behavior.

Primary vs User-defined context

HIP has two different types of context, the Primary context, which is usable by all threads on a given process for a given device, and the aforementioned custom contexts. HIP documentation, and performance analysis, indicates it is recommended to use Primary context whenever possible. Primary context is used as well by the HIP Runtime API. For PI applications to interop with HIP Runtime API, they have to use the primary context - and make that active in the thread. The _pi_context object can be constructed with a kind parameter that allows to construct a Primary or user-defined context, so that the PI object interface is always the same.

Destructor callback

Required to implement CP023, SYCL Extended Context Destruction, the PI Context can store a number of callback functions that will be called upon destruction of the PI Context. See proposal for details.

Definition at line 170 of file pi_cuda.hpp.

Member Typedef Documentation

◆ native_type [1/2]

using _pi_context::native_type = hipCtx_t

Definition at line 148 of file pi_hip.hpp.

◆ native_type [2/2]

using _pi_context::native_type = CUcontext

Definition at line 179 of file pi_cuda.hpp.

Member Enumeration Documentation

◆ kind

enum _pi_context::kind

strong

Enumerator
primary
user_defined

Definition at line 150 of file pi_hip.hpp.

Constructor & Destructor Documentation

◆ _pi_context() [1/4]

_pi_context::_pi_context ( _pi_device * devId )

inline

Definition at line 185 of file pi_cuda.hpp.

References _pi_device::get_context().

◆ ~_pi_context() [1/2]

_pi_context::~_pi_context ( )

inline

Definition at line 190 of file pi_cuda.hpp.

References cuda_piDeviceRelease(), and deviceId_.

◆ _pi_context() [2/4]

_pi_context::_pi_context ( pi_device ArgDevice )

inline

Definition at line 95 of file pi_esimd_emulator.hpp.

◆ _pi_context() [3/4]

_pi_context::_pi_context	(	kind	k,
		hipCtx_t	ctxt,
		_pi_device *	devId
	)

inline

Definition at line 155 of file pi_hip.hpp.

◆ ~_pi_context() [2/2]

_pi_context::~_pi_context ( )

inline

Definition at line 161 of file pi_hip.hpp.

References deviceId_, and hip_piDeviceRelease().

◆ _pi_context() [4/4]

_pi_context::_pi_context	(	ze_context_handle_t	ZeContext,
		pi_uint32	NumDevices,
		const pi_device *	Devs,
		bool	OwnZeContext
	)

inline

Definition at line 208 of file pi_level_zero.hpp.

References ZeContext.

Member Function Documentation

◆ addEventToContextCache()

void _pi_context::addEventToContextCache ( pi_event Event )

Definition at line 4657 of file pi_level_zero.cpp.

References _pi_event::isHostVisible(), and _pi_event::isProfilingEnabled().

Referenced by piEventReleaseInternal().

◆ checkSurfaceArgument()

bool _pi_context::checkSurfaceArgument	(	pi_mem_flags	Flags,
		void *	HostPtr
	)

Definition at line 915 of file pi_esimd_emulator.cpp.

References PI_MEM_FLAGS_HOST_PTR_COPY, PI_MEM_FLAGS_HOST_PTR_USE, and PiTrace().

Referenced by piMemBufferCreate(), and piMemImageCreate().

◆ decrement_reference_count() [1/2]

pi_uint32 _pi_context::decrement_reference_count ( )

inlinenoexcept

Definition at line 184 of file pi_hip.hpp.

References refCount_.

◆ decrement_reference_count() [2/2]

pi_uint32 _pi_context::decrement_reference_count ( )

inlinenoexcept

Definition at line 211 of file pi_cuda.hpp.

References refCount_.

Referenced by cuda_piContextRelease(), and hip_piContextRelease().

◆ decrementUnreleasedEventsInPool()

pi_result _pi_context::decrementUnreleasedEventsInPool ( pi_event Event )

Definition at line 282 of file pi_level_zero.cpp.

References sycl::_V1::detail::pi::die(), _pi_event::isHostVisible(), _pi_event::isProfilingEnabled(), and _pi_event::ZeEventPool.

Referenced by piEventReleaseInternal().

◆ finalize()

pi_result _pi_context::finalize ( )

Definition at line 601 of file pi_level_zero.cpp.

References ZE_CALL, ZeCommandListCacheMutex, ZeCommandListInit, ZeComputeCommandListCache, and ZeCopyCommandListCache.

Referenced by ContextReleaseHelper().

◆ get() [1/2]

native_type _pi_context::get ( ) const

inlinenoexcept

Definition at line 178 of file pi_hip.hpp.

References hipContext_.

◆ get() [2/2]

native_type _pi_context::get ( ) const

inlinenoexcept

Definition at line 207 of file pi_cuda.hpp.

References cuContext_.

Referenced by cuda_piextContextGetNativeHandle(), hip_piContextRelease(), and hip_piextContextGetNativeHandle().

◆ get_device() [1/2]

pi_device _pi_context::get_device ( ) const

inlinenoexcept

Definition at line 176 of file pi_hip.hpp.

References deviceId_.

◆ get_device() [2/2]

pi_device _pi_context::get_device ( ) const

inlinenoexcept

Definition at line 205 of file pi_cuda.hpp.

References deviceId_.

Referenced by cuda_piContextGetInfo(), cuda_piextGetDeviceFunctionPointer(), cuda_piextQueueCreateWithNativeHandle(), cuda_piextUSMEnqueueMemAdvise(), cuda_piextUSMEnqueuePrefetch(), cuda_piProgramCreateWithBinary(), cuda_piQueueCreate(), hip_piContextGetInfo(), hip_piContextRelease(), hip_piextGetDeviceFunctionPointer(), hip_piextUSMEnqueuePrefetch(), hip_piProgramCreateWithBinary(), and hip_piQueueCreate().

◆ get_reference_count() [1/2]

pi_uint32 _pi_context::get_reference_count ( ) const

inlinenoexcept

Definition at line 186 of file pi_hip.hpp.

References refCount_.

◆ get_reference_count() [2/2]

pi_uint32 _pi_context::get_reference_count ( ) const

inlinenoexcept

Definition at line 213 of file pi_cuda.hpp.

References refCount_.

Referenced by cuda_piContextGetInfo(), cuda_piContextRetain(), hip_piContextGetInfo(), and hip_piContextRetain().

◆ getAvailableCommandList()

pi_result _pi_context::getAvailableCommandList	(	pi_queue	Queue,
		pi_command_list_ptr_t &	CommandList,
		bool	UseCopyEngine,
		bool	AllowBatching = `false`,
		ze_command_queue_handle_t *	ForcedCmdQueue = `nullptr`
	)

Definition at line 1100 of file pi_level_zero.cpp.

References CleanupEventListFromResetCmdList(), _pi_queue::CommandListMap, _pi_queue::ComputeCommandBatch, _pi_queue::Context, _pi_queue::CopyCommandBatch, _pi_queue::createCommandList(), _pi_queue::Device, _pi_queue::executeOpenCommandList(), _pi_queue::pi_queue_group_t::getImmCmdList(), _pi_queue::getQueueGroup(), _pi_queue::pi_queue_group_t::getZeQueue(), _pi_queue::hasOpenCommandList(), ImmCmdListsEventCleanupThreshold, _pi_queue::insertActiveBarriers(), _pi_queue::insertStartBarrierIfDiscardEventsMode(), _pi_queue::command_batch::OpenCommandList, PI_CALL, _pi_queue::resetCommandList(), ZE_CALL, ZE_CALL_NOCHECK, ZeCommandListCacheMutex, ZeComputeCommandListCache, and ZeCopyCommandListCache.

Referenced by enqueueMemCopyHelper(), enqueueMemCopyRectHelper(), enqueueMemFillHelper(), enqueueMemImageCommandHelper(), piEnqueueEventsWait(), piEnqueueEventsWaitWithBarrier(), piEnqueueKernelLaunch(), piEnqueueMemBufferMap(), piEnqueueMemUnmap(), piextUSMEnqueueMemAdvise(), and piextUSMEnqueuePrefetch().

◆ getEventFromContextCache()

pi_event _pi_context::getEventFromContextCache	(	bool	HostVisible,
		bool	WithProfiling
	)

Definition at line 4642 of file pi_level_zero.cpp.

References _pi_event::reset().

Referenced by EventCreate().

◆ getFreeSlotInExistingOrNewPool()

pi_result _pi_context::getFreeSlotInExistingOrNewPool	(	ze_event_pool_handle_t &	Pool,
		size_t &	Index,
		bool	HostVisible,
		bool	ProfilingEnabled
	)

Definition at line 223 of file pi_level_zero.cpp.

References Devices, sycl::_V1::detail::for_each(), ZE_CALL, ZeContext, and zePrint().

Referenced by EventCreate().

◆ getPlatform()

pi_platform _pi_context::getPlatform ( ) const

Definition at line 211 of file pi_level_zero.cpp.

References Devices.

Referenced by ContextReleaseHelper(), _pi_buffer::free(), piContextRelease(), piextMemCreateWithNativeHandle(), piextUSMFree(), piextUSMGetMemAllocInfo(), piextUSMHostAlloc(), piMemBufferCreate(), piSamplerCreate(), USMFreeHelper(), ZeHostMemAllocHelper(), and ZeMemFreeHelper().

◆ increment_reference_count() [1/2]

pi_uint32 _pi_context::increment_reference_count ( )

inlinenoexcept

Definition at line 182 of file pi_hip.hpp.

References refCount_.

◆ increment_reference_count() [2/2]

pi_uint32 _pi_context::increment_reference_count ( )

inlinenoexcept

Definition at line 209 of file pi_cuda.hpp.

References refCount_.

Referenced by cuda_piContextRetain(), and hip_piContextRetain().

◆ initialize()

pi_result _pi_context::initialize ( )

Definition at line 512 of file pi_level_zero.cpp.

References usm_settings::USMAllocatorConfig::Configs, Device, DeviceMemAllocContexts, Devices, getRangeOfAllowedCopyEngines(), usm_settings::Host, HostMemAllocContext, sycl::_V1::detail::make_tuple(), usm_settings::Shared, SharedMemAllocContexts, usm_settings::SharedReadOnly, SharedReadOnlyMemAllocContexts, SingleRootDevice, ZE_CALL, ZeCommandListInit, and ZeContext.

◆ invoke_extended_deleters() [1/2]

void _pi_context::invoke_extended_deleters ( )

inline

Definition at line 163 of file pi_hip.hpp.

◆ invoke_extended_deleters() [2/2]

void _pi_context::invoke_extended_deleters ( )

inline

Definition at line 192 of file pi_cuda.hpp.

Referenced by cuda_piContextRelease(), and hip_piContextRelease().

◆ is_primary()

bool _pi_context::is_primary ( ) const

inlinenoexcept

Definition at line 180 of file pi_hip.hpp.

References kind_, and primary.

Referenced by hip_piContextRelease().

◆ isValidDevice()

bool _pi_context::isValidDevice ( pi_device Device ) const

Definition at line 213 of file pi_level_zero.cpp.

References Device, and Devices.

Referenced by piextMemCreateWithNativeHandle(), piextQueueCreate(), piProgramBuild(), and piProgramLink().

◆ set_extended_deleter() [1/2]

void _pi_context::set_extended_deleter	(	pi_context_extended_deleter	function,
		void *	user_data
	)

inline

Definition at line 170 of file pi_hip.hpp.

◆ set_extended_deleter() [2/2]

void _pi_context::set_extended_deleter	(	pi_context_extended_deleter	function,
		void *	user_data
	)

inline

Definition at line 199 of file pi_cuda.hpp.

Referenced by cuda_piextContextSetExtendedDeleter(), and hip_piextContextSetExtendedDeleter().

Member Data Documentation

◆ Addr2CmBufferSVM

std::unordered_map<void *, cm_support::CmBufferSVM *> _pi_context::Addr2CmBufferSVM

Definition at line 102 of file pi_esimd_emulator.hpp.

Referenced by piContextRelease(), piextUSMFree(), and piextUSMSharedAlloc().

◆ Addr2CmBufferSVMLock

std::mutex _pi_context::Addr2CmBufferSVMLock

Definition at line 104 of file pi_esimd_emulator.hpp.

Referenced by piContextRelease(), piextUSMFree(), and piextUSMSharedAlloc().

◆ cuContext_

native_type _pi_context::cuContext_

Definition at line 181 of file pi_cuda.hpp.

Referenced by get().

◆ Device

pi_device _pi_context::Device

Definition at line 98 of file pi_esimd_emulator.hpp.

Referenced by initialize(), isValidDevice(), piContextRelease(), piextUSMFree(), piextUSMSharedAlloc(), piMemBufferCreate(), piMemImageCreate(), and piQueueCreate().

◆ deviceId_

_pi_device * _pi_context::deviceId_

Definition at line 182 of file pi_cuda.hpp.

Referenced by cuda_piProgramGetInfo(), get_device(), hip_piProgramGetInfo(), and ~_pi_context().

◆ DeviceMemAllocContexts

std::unordered_map<ze_device_handle_t, USMAllocContext> _pi_context::DeviceMemAllocContexts

Definition at line 323 of file pi_level_zero.hpp.

Referenced by initialize(), piextUSMDeviceAlloc(), and USMFreeHelper().

◆ Devices

const std::vector<pi_device> _pi_context::Devices

Definition at line 239 of file pi_level_zero.hpp.

Referenced by getFreeSlotInExistingOrNewPool(), getPlatform(), _pi_buffer::getZeHandle(), initialize(), isValidDevice(), piContextGetInfo(), piEventGetProfilingInfo(), piMemBufferCreate(), piMemImageCreate(), piProgramGetInfo(), piSamplerCreate(), and USMAllocationMakeResident().

◆ hipContext_

native_type _pi_context::hipContext_

Definition at line 151 of file pi_hip.hpp.

Referenced by get().

◆ HostMemAllocContext

std::unique_ptr<USMAllocContext> _pi_context::HostMemAllocContext

Definition at line 335 of file pi_level_zero.hpp.

Referenced by initialize(), piextUSMHostAlloc(), and USMFreeHelper().

◆ ImmediateCommandListMutex

pi_mutex _pi_context::ImmediateCommandListMutex

Definition at line 264 of file pi_level_zero.hpp.

Referenced by _pi_buffer::getZeHandle(), piextMemCreateWithNativeHandle(), piMemBufferCreate(), and piMemImageCreate().

◆ kind_

enum _pi_context::kind _pi_context::kind_

Referenced by is_primary().

◆ MemAllocs

std::unordered_map<void *, MemAllocRecord> _pi_context::MemAllocs

Definition at line 342 of file pi_level_zero.hpp.

Referenced by piextMemCreateWithNativeHandle(), piextUSMDeviceAlloc(), piextUSMHostAlloc(), piextUSMSharedAlloc(), USMFreeHelper(), ZeDeviceMemAllocHelper(), ZeHostMemAllocHelper(), and ZeMemFreeHelper().

◆ OwnZeContext

bool _pi_context::OwnZeContext

Definition at line 234 of file pi_level_zero.hpp.

Referenced by ContextReleaseHelper().

◆ refCount_

std::atomic_uint32_t _pi_context::refCount_

Definition at line 183 of file pi_cuda.hpp.

Referenced by decrement_reference_count(), get_reference_count(), and increment_reference_count().

◆ SharedMemAllocContexts

std::unordered_map<ze_device_handle_t, USMAllocContext> _pi_context::SharedMemAllocContexts

Definition at line 325 of file pi_level_zero.hpp.

Referenced by initialize(), piextUSMSharedAlloc(), and USMFreeHelper().

◆ SharedReadOnlyAllocs

std::unordered_set<void *> _pi_context::SharedReadOnlyAllocs

Definition at line 332 of file pi_level_zero.hpp.

Referenced by piextUSMSharedAlloc(), and USMFreeHelper().

◆ SharedReadOnlyMemAllocContexts

std::unordered_map<ze_device_handle_t, USMAllocContext> _pi_context::SharedReadOnlyMemAllocContexts

Definition at line 327 of file pi_level_zero.hpp.

Referenced by initialize(), piextUSMSharedAlloc(), and USMFreeHelper().

◆ SingleRootDevice

const pi_device _pi_context::SingleRootDevice = nullptr

Definition at line 249 of file pi_level_zero.hpp.

Referenced by _pi_buffer::getZeHandle(), initialize(), and piMemImageCreate().

◆ ZeCommandListCacheMutex

pi_mutex _pi_context::ZeCommandListCacheMutex

Definition at line 268 of file pi_level_zero.hpp.

Referenced by finalize(), getAvailableCommandList(), and _pi_queue::resetCommandList().

◆ ZeCommandListInit

ze_command_list_handle_t _pi_context::ZeCommandListInit

Definition at line 259 of file pi_level_zero.hpp.

Referenced by finalize(), _pi_buffer::getZeHandle(), initialize(), piextMemCreateWithNativeHandle(), piMemBufferCreate(), and piMemImageCreate().

◆ ZeComputeCommandListCache

std::unordered_map<ze_device_handle_t, std::list<ze_command_list_handle_t> > _pi_context::ZeComputeCommandListCache

Definition at line 278 of file pi_level_zero.hpp.

Referenced by finalize(), getAvailableCommandList(), and _pi_queue::resetCommandList().

◆ ZeContext

◆ ZeCopyCommandListCache

std::unordered_map<ze_device_handle_t, std::list<ze_command_list_handle_t> > _pi_context::ZeCopyCommandListCache

Definition at line 280 of file pi_level_zero.hpp.

Referenced by finalize(), getAvailableCommandList(), and _pi_queue::resetCommandList().

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

plugins/cuda/pi_cuda.hpp
plugins/hip/pi_hip.hpp
plugins/esimd_emulator/pi_esimd_emulator.hpp
plugins/level_zero/pi_level_zero.hpp
plugins/esimd_emulator/pi_esimd_emulator.cpp
plugins/level_zero/pi_level_zero.cpp

Classes

Public Types

Public Member Functions

Public Attributes

Detailed Description

Member Typedef Documentation

◆ native_type [1/2]

◆ native_type [2/2]

Member Enumeration Documentation

◆ kind

Constructor & Destructor Documentation

◆ _pi_context() [1/4]

◆ ~_pi_context() [1/2]

◆ _pi_context() [2/4]

◆ _pi_context() [3/4]

◆ ~_pi_context() [2/2]

◆ _pi_context() [4/4]

Member Function Documentation

◆ addEventToContextCache()

◆ checkSurfaceArgument()

◆ decrement_reference_count() [1/2]

◆ decrement_reference_count() [2/2]

◆ decrementUnreleasedEventsInPool()

◆ finalize()

◆ get() [1/2]

◆ get() [2/2]

◆ get_device() [1/2]

◆ get_device() [2/2]

◆ get_reference_count() [1/2]

◆ get_reference_count() [2/2]

◆ getAvailableCommandList()

◆ getEventFromContextCache()

◆ getFreeSlotInExistingOrNewPool()

◆ getPlatform()

◆ increment_reference_count() [1/2]

◆ increment_reference_count() [2/2]

◆ initialize()

◆ invoke_extended_deleters() [1/2]

◆ invoke_extended_deleters() [2/2]

◆ is_primary()

◆ isValidDevice()

◆ set_extended_deleter() [1/2]

◆ set_extended_deleter() [2/2]

Member Data Documentation

◆ Addr2CmBufferSVM

◆ Addr2CmBufferSVMLock

◆ cuContext_

◆ Device

◆ deviceId_

◆ DeviceMemAllocContexts

◆ Devices

◆ hipContext_

◆ HostMemAllocContext

◆ ImmediateCommandListMutex

◆ kind_

◆ MemAllocs

◆ OwnZeContext

◆ refCount_

◆ SharedMemAllocContexts

◆ SharedReadOnlyAllocs

◆ SharedReadOnlyMemAllocContexts

◆ SingleRootDevice

◆ ZeCommandListCacheMutex

◆ ZeCommandListInit

◆ ZeComputeCommandListCache

◆ ZeContext

◆ ZeCopyCommandListCache