sycl::_V1::detail::usm Namespace Reference

Functions
void *	alignedAlloc (size_t Alignment, size_t Bytes, const context &Ctxt, const device &Dev, sycl::usm::alloc Kind, const code_location &CL)
void *	alignedAllocHost (size_t Alignment, size_t Bytes, const context &Ctxt, sycl::usm::alloc Kind, const code_location &CL)
void	free (void *Ptr, const context &Ctxt, const code_location &CL)
void *	alignedAllocHost (size_t Alignment, size_t Size, const context &Ctxt, alloc Kind, const property_list &PropList, const detail::code_location &CodeLoc)
void *	alignedAllocInternal (size_t Alignment, size_t Size, const context_impl *CtxImpl, const device_impl *DevImpl, alloc Kind, const property_list &PropList)
void *	alignedAlloc (size_t Alignment, size_t Size, const context &Ctxt, const device &Dev, alloc Kind, const property_list &PropList, const detail::code_location &CodeLoc)
void	freeInternal (void *Ptr, const context_impl *CtxImpl)

Function Documentation

alignedAlloc() [1/2]

void* sycl::_V1::detail::usm::alignedAlloc	(	size_t	Alignment,
		size_t	Bytes,
		const context &	Ctxt,
		const device &	Dev,
		sycl::usm::alloc	Kind,
		const code_location &	CL
	)

Referenced by sycl::_V1::detail::aligned_allocator< T >::allocate().

alignedAlloc() [2/2]

void* sycl::_V1::detail::usm::alignedAlloc	(	size_t	Alignment,
		size_t	Size,
		const context &	Ctxt,
		const device &	Dev,
		alloc	Kind,
		const property_list &	PropList,
		const detail::code_location &	CodeLoc
	)

Definition at line 228 of file usm_impl.cpp.

References alignedAllocInternal(), sycl::_V1::ext::oneapi::experimental::detail::Alignment, std::get(), sycl::_V1::device::get_info(), sycl::_V1::detail::getSyclObjImpl(), and sycl::_V1::detail::SYCL_MEM_ALLOC_STREAM_NAME.

Referenced by sycl::_V1::aligned_alloc(), sycl::_V1::aligned_alloc_device(), sycl::_V1::aligned_alloc_shared(), sycl::_V1::malloc(), sycl::_V1::malloc_device(), and sycl::_V1::malloc_shared().

alignedAllocHost() [1/2]

void* sycl::_V1::detail::usm::alignedAllocHost	(	size_t	Alignment,
		size_t	Bytes,
		const context &	Ctxt,
		sycl::usm::alloc	Kind,
		const code_location &	CL
	)

alignedAllocHost() [2/2]

void* sycl::_V1::detail::usm::alignedAllocHost	(	size_t	Alignment,
		size_t	Size,
		const context &	Ctxt,
		alloc	Kind,
		const property_list &	PropList,
		const detail::code_location &	CodeLoc
	)

Definition at line 41 of file usm_impl.cpp.

References sycl::_V1::ext::oneapi::experimental::detail::Alignment, sycl::_V1::detail::aligned_allocator< T >::allocate(), sycl::_V1::ext::oneapi::experimental::buffer_location, sycl::_V1::detail::plugin::call_nocheck(), sycl::_V1::context::get_platform(), sycl::_V1::property_list::get_property(), sycl::_V1::detail::getSyclObjImpl(), sycl::_V1::property_list::has_property(), PI_MEM_USM_ALLOC_BUFFER_LOCATION, piextUSMHostAlloc(), and sycl::_V1::detail::SYCL_MEM_ALLOC_STREAM_NAME.

Referenced by sycl::_V1::aligned_alloc(), sycl::_V1::aligned_alloc_host(), sycl::_V1::malloc(), and sycl::_V1::malloc_host().

alignedAllocInternal()

void * sycl::_V1::detail::usm::alignedAllocInternal	(	size_t	Alignment,
		size_t	Size,
		const context_impl *	CtxImpl,
		const device_impl *	DevImpl,
		alloc	Kind,
		const property_list &	PropList
	)

Definition at line 125 of file usm_impl.cpp.

References sycl::_V1::ext::oneapi::experimental::detail::Alignment, sycl::_V1::detail::aligned_allocator< T >::allocate(), sycl::_V1::ext::oneapi::experimental::buffer_location, sycl::_V1::detail::plugin::call_nocheck(), sycl::_V1::property_list::get_property(), sycl::_V1::detail::device_impl::getHandleRef(), sycl::_V1::detail::context_impl::getHandleRef(), sycl::_V1::detail::context_impl::getPlugin(), sycl::_V1::detail::device_impl::has_extension(), sycl::_V1::property_list::has_property(), sycl::_V1::detail::context_impl::is_host(), PI_MEM_ALLOC_DEVICE_READ_ONLY, PI_MEM_ALLOC_FLAGS, PI_MEM_USM_ALLOC_BUFFER_LOCATION, piextUSMDeviceAlloc(), and piextUSMSharedAlloc().

Referenced by alignedAlloc(), and sycl::_V1::detail::DeviceGlobalMapEntry::getOrAllocateDeviceGlobalUSM().

free()

void sycl::_V1::detail::usm::free	(	void *	Ptr,
		const context &	Ctxt,
		const code_location &	CL
	)

Definition at line 267 of file usm_impl.cpp.

References sycl::_V1::free(), freeInternal(), std::get(), sycl::_V1::detail::getSyclObjImpl(), and sycl::_V1::detail::SYCL_MEM_ALLOC_STREAM_NAME.

Referenced by sycl::_V1::detail::OSUtil::alignedFree(), sycl::_V1::usm_allocator< T, AllocKind, Alignment >::deallocate(), _pi_buffer::free(), sycl::_V1::detail::reduction_impl_algo< T, BinaryOperation, Dims, Extent, ExplicitIdentity, RedOutVar >::getGroupsCounterAccDiscrete(), _pi_buffer::getZeHandle(), and _pi_mem::mem_::buffer_mem_::unmap().

freeInternal()

void sycl::_V1::detail::usm::freeInternal	(	void *	Ptr,
		const context_impl *	CtxImpl
	)

Definition at line 254 of file usm_impl.cpp.

References sycl::_V1::detail::plugin::call(), sycl::_V1::detail::context_impl::getHandleRef(), sycl::_V1::detail::context_impl::getPlugin(), sycl::_V1::detail::context_impl::is_host(), and piextUSMFree().

Referenced by free(), and sycl::_V1::detail::DeviceGlobalMapEntry::removeAssociatedResources().