DPC++ Runtime
Runtime libraries for oneAPI DPC++
usm_impl.cpp File Reference
#include <detail/queue_impl.hpp>
#include <detail/usm/usm_impl.hpp>
#include <sycl/context.hpp>
#include <sycl/detail/aligned_allocator.hpp>
#include <sycl/detail/os_util.hpp>
#include <sycl/detail/pi.hpp>
#include <sycl/device.hpp>
#include <sycl/ext/intel/experimental/usm_properties.hpp>
#include <sycl/ext/oneapi/memcpy2d.hpp>
#include <sycl/usm.hpp>
#include <array>
#include <cassert>
#include <cstdlib>
#include <memory>
Include dependency graph for usm_impl.cpp:

Go to the source code of this file.

Namespaces

 sycl
 
 sycl::_V1
 
 sycl::_V1::detail
 
 sycl::_V1::detail::usm
 
 sycl::_V1::ext
 
 sycl::_V1::ext::oneapi
 
 sycl::_V1::ext::oneapi::experimental
 

Typedefs

using sycl::_V1::alloc = sycl::usm::alloc
 

Functions

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)
 
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)
 
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)
 
void sycl::_V1::detail::usm::freeInternal (void *Ptr, const context_impl *CtxImpl)
 
void sycl::_V1::detail::usm::free (void *Ptr, const context &Ctxt, const code_location &CL)
 
void * sycl::_V1::malloc_device (size_t size, const device &dev, const context &ctxt, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_device (size_t size, const device &dev, const context &ctxt, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_device (size_t size, const queue &q, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_device (size_t size, const queue &q, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_device (size_t alignment, size_t size, const device &dev, const context &ctxt, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_device (size_t alignment, size_t size, const device &dev, const context &ctxt, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_device (size_t alignment, size_t size, const queue &q, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_device (size_t alignment, size_t size, const queue &q, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void sycl::_V1::free (void *ptr, const context &ctxt, const detail::code_location &CodeLoc=detail::code_location::current())
 
void sycl::_V1::free (void *ptr, const queue &q, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_host (size_t size, const context &ctxt, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_host (size_t size, const context &ctxt, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_host (size_t size, const queue &q, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_host (size_t size, const queue &q, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_shared (size_t size, const device &dev, const context &ctxt, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_shared (size_t size, const device &dev, const context &ctxt, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_shared (size_t size, const queue &q, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc_shared (size_t size, const queue &q, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_host (size_t alignment, size_t size, const context &ctxt, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_host (size_t alignment, size_t size, const context &ctxt, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_host (size_t alignment, size_t size, const queue &q, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_host (size_t alignment, size_t size, const queue &q, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_shared (size_t alignment, size_t size, const device &dev, const context &ctxt, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_shared (size_t alignment, size_t size, const device &dev, const context &ctxt, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_shared (size_t alignment, size_t size, const queue &q, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::aligned_alloc_shared (size_t alignment, size_t size, const queue &q, const property_list &propList, const detail::code_location &CodeLoc=detail::code_location::current())
 
void * sycl::_V1::malloc (size_t Size, const device &Dev, const context &Ctxt, alloc Kind, const property_list &PropList, const detail::code_location &CodeLoc)
 
void * sycl::_V1::malloc (size_t Size, const device &Dev, const context &Ctxt, alloc Kind, const detail::code_location &CodeLoc)
 
void * sycl::_V1::malloc (size_t Size, const queue &Q, alloc Kind, const detail::code_location &CodeLoc)
 
void * sycl::_V1::malloc (size_t Size, const queue &Q, alloc Kind, const property_list &PropList, const detail::code_location &CodeLoc)
 
void * sycl::_V1::aligned_alloc (size_t Alignment, size_t Size, const device &Dev, const context &Ctxt, alloc Kind, const detail::code_location &CodeLoc)
 
void * sycl::_V1::aligned_alloc (size_t Alignment, size_t Size, const device &Dev, const context &Ctxt, alloc Kind, const property_list &PropList, const detail::code_location &CodeLoc)
 
void * sycl::_V1::aligned_alloc (size_t Alignment, size_t Size, const queue &Q, alloc Kind, const detail::code_location &CodeLoc)
 
void * sycl::_V1::aligned_alloc (size_t Alignment, size_t Size, const queue &Q, alloc Kind, const property_list &PropList, const detail::code_location &CodeLoc)
 
usm::alloc sycl::_V1::get_pointer_type (const void *ptr, const context &ctxt)
 Query the allocation type from a USM pointer. More...
 
device sycl::_V1::get_pointer_device (const void *ptr, const context &ctxt)
 Queries the device against which the pointer was allocated Throws an exception with errc::invalid error code if ptr is a host allocation. More...
 
static void sycl::_V1::prepare_for_usm_device_copy (const void *Ptr, size_t Size, const context &Ctxt)
 
static void sycl::_V1::release_from_usm_device_copy (const void *Ptr, const context &Ctxt)
 
void sycl::_V1::ext::oneapi::experimental::prepare_for_device_copy (const void *Ptr, size_t Size, const context &Context)
 
void sycl::_V1::ext::oneapi::experimental::prepare_for_device_copy (const void *Ptr, size_t Size, const queue &Queue)
 
void sycl::_V1::ext::oneapi::experimental::release_from_device_copy (const void *Ptr, const context &Context)
 
void sycl::_V1::ext::oneapi::experimental::release_from_device_copy (const void *Ptr, const queue &Queue)