DPC++ Runtime
Runtime libraries for oneAPI DPC++
Static Public Member Functions | List of all members
sycl::_V1::detail::MemoryManager Class Reference

#include <detail/memory_manager.hpp>

Static Public Member Functions

static void release (ContextImplPtr TargetContext, SYCLMemObjI *MemObj, void *MemAllocation, std::vector< EventImplPtr > DepEvents, ur_event_handle_t &OutEvent)
 
static void * allocate (ContextImplPtr TargetContext, SYCLMemObjI *MemObj, bool InitFromUserData, void *HostPtr, std::vector< EventImplPtr > DepEvents, ur_event_handle_t &OutEvent)
 
static void * allocateMemSubBuffer (ContextImplPtr TargetContext, void *ParentMemObj, size_t ElemSize, size_t Offset, range< 3 > Range, std::vector< EventImplPtr > DepEvents, ur_event_handle_t &OutEvent)
 
static void * allocateMemBuffer (ContextImplPtr TargetContext, SYCLMemObjI *MemObj, void *UserPtr, bool HostPtrReadOnly, size_t Size, const EventImplPtr &InteropEvent, const ContextImplPtr &InteropContext, const sycl::property_list &PropsList, ur_event_handle_t &OutEventToWait)
 
static void * allocateMemImage (ContextImplPtr TargetContext, SYCLMemObjI *MemObj, void *UserPtr, bool HostPtrReadOnly, size_t Size, const ur_image_desc_t &Desc, const ur_image_format_t &Format, const EventImplPtr &InteropEvent, const ContextImplPtr &InteropContext, const sycl::property_list &PropsList, ur_event_handle_t &OutEventToWait)
 
static void releaseMemObj (ContextImplPtr TargetContext, SYCLMemObjI *MemObj, void *MemAllocation, void *UserPtr)
 
static void * allocateHostMemory (SYCLMemObjI *MemObj, void *UserPtr, bool HostPtrReadOnly, size_t Size, const sycl::property_list &PropsList)
 
static void * allocateInteropMemObject (ContextImplPtr TargetContext, void *UserPtr, const EventImplPtr &InteropEvent, const ContextImplPtr &InteropContext, const sycl::property_list &PropsList, ur_event_handle_t &OutEventToWait)
 
static void * allocateImageObject (ContextImplPtr TargetContext, void *UserPtr, bool HostPtrReadOnly, const ur_image_desc_t &Desc, const ur_image_format_t &Format, const sycl::property_list &PropsList)
 
static void * allocateBufferObject (ContextImplPtr TargetContext, void *UserPtr, bool HostPtrReadOnly, const size_t Size, const sycl::property_list &PropsList)
 
static void copy (SYCLMemObjI *SYCLMemObj, void *SrcMem, QueueImplPtr SrcQueue, unsigned int DimSrc, sycl::range< 3 > SrcSize, sycl::range< 3 > SrcAccessRange, sycl::id< 3 > SrcOffset, unsigned int SrcElemSize, void *DstMem, QueueImplPtr TgtQueue, unsigned int DimDst, sycl::range< 3 > DstSize, sycl::range< 3 > DstAccessRange, sycl::id< 3 > DstOffset, unsigned int DstElemSize, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t &OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void fill (SYCLMemObjI *SYCLMemObj, void *Mem, QueueImplPtr Queue, size_t PatternSize, const unsigned char *Pattern, unsigned int Dim, sycl::range< 3 > Size, sycl::range< 3 > AccessRange, sycl::id< 3 > AccessOffset, unsigned int ElementSize, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t &OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void * map (SYCLMemObjI *SYCLMemObj, void *Mem, QueueImplPtr Queue, access::mode AccessMode, unsigned int Dim, sycl::range< 3 > Size, sycl::range< 3 > AccessRange, sycl::id< 3 > AccessOffset, unsigned int ElementSize, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t &OutEvent)
 
static void unmap (SYCLMemObjI *SYCLMemObj, void *Mem, QueueImplPtr Queue, void *MappedPtr, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t &OutEvent)
 
static void copy_usm (const void *SrcMem, QueueImplPtr Queue, size_t Len, void *DstMem, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void fill_usm (void *DstMem, QueueImplPtr Queue, size_t Len, const std::vector< unsigned char > &Pattern, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void prefetch_usm (void *Ptr, QueueImplPtr Queue, size_t Len, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void advise_usm (const void *Ptr, QueueImplPtr Queue, size_t Len, ur_usm_advice_flags_t Advice, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void copy_2d_usm (const void *SrcMem, size_t SrcPitch, QueueImplPtr Queue, void *DstMem, size_t DstPitch, size_t Width, size_t Height, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void fill_2d_usm (void *DstMem, QueueImplPtr Queue, size_t Pitch, size_t Width, size_t Height, const std::vector< unsigned char > &Pattern, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void memset_2d_usm (void *DstMem, QueueImplPtr Queue, size_t Pitch, size_t Width, size_t Height, char Value, std::vector< ur_event_handle_t > DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void copy_to_device_global (const void *DeviceGlobalPtr, bool IsDeviceImageScoped, QueueImplPtr Queue, size_t NumBytes, size_t Offset, const void *SrcMem, const std::vector< ur_event_handle_t > &DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void copy_from_device_global (const void *DeviceGlobalPtr, bool IsDeviceImageScoped, QueueImplPtr Queue, size_t NumBytes, size_t Offset, void *DstMem, const std::vector< ur_event_handle_t > &DepEvents, ur_event_handle_t *OutEvent, const detail::EventImplPtr &OutEventImpl)
 
static void ext_oneapi_copyD2D_cmd_buffer (sycl::detail::ContextImplPtr Context, ur_exp_command_buffer_handle_t CommandBuffer, SYCLMemObjI *SYCLMemObj, void *SrcMem, unsigned int DimSrc, sycl::range< 3 > SrcSize, sycl::range< 3 > SrcAccessRange, sycl::id< 3 > SrcOffset, unsigned int SrcElemSize, void *DstMem, unsigned int DimDst, sycl::range< 3 > DstSize, sycl::range< 3 > DstAccessRange, sycl::id< 3 > DstOffset, unsigned int DstElemSize, std::vector< ur_exp_command_buffer_sync_point_t > Deps, ur_exp_command_buffer_sync_point_t *OutSyncPoint)
 
static void ext_oneapi_copyD2H_cmd_buffer (sycl::detail::ContextImplPtr Context, ur_exp_command_buffer_handle_t CommandBuffer, SYCLMemObjI *SYCLMemObj, void *SrcMem, unsigned int DimSrc, sycl::range< 3 > SrcSize, sycl::range< 3 > SrcAccessRange, sycl::id< 3 > SrcOffset, unsigned int SrcElemSize, char *DstMem, unsigned int DimDst, sycl::range< 3 > DstSize, sycl::id< 3 > DstOffset, unsigned int DstElemSize, std::vector< ur_exp_command_buffer_sync_point_t > Deps, ur_exp_command_buffer_sync_point_t *OutSyncPoint)
 
static void ext_oneapi_copyH2D_cmd_buffer (sycl::detail::ContextImplPtr Context, ur_exp_command_buffer_handle_t CommandBuffer, SYCLMemObjI *SYCLMemObj, char *SrcMem, unsigned int DimSrc, sycl::range< 3 > SrcSize, sycl::id< 3 > SrcOffset, unsigned int SrcElemSize, void *DstMem, unsigned int DimDst, sycl::range< 3 > DstSize, sycl::range< 3 > DstAccessRange, sycl::id< 3 > DstOffset, unsigned int DstElemSize, std::vector< ur_exp_command_buffer_sync_point_t > Deps, ur_exp_command_buffer_sync_point_t *OutSyncPoint)
 
static void ext_oneapi_copy_usm_cmd_buffer (ContextImplPtr Context, const void *SrcMem, ur_exp_command_buffer_handle_t CommandBuffer, size_t Len, void *DstMem, std::vector< ur_exp_command_buffer_sync_point_t > Deps, ur_exp_command_buffer_sync_point_t *OutSyncPoint)
 
static void ext_oneapi_fill_usm_cmd_buffer (sycl::detail::ContextImplPtr Context, ur_exp_command_buffer_handle_t CommandBuffer, void *DstMem, size_t Len, const std::vector< unsigned char > &Pattern, std::vector< ur_exp_command_buffer_sync_point_t > Deps, ur_exp_command_buffer_sync_point_t *OutSyncPoint)
 
static void ext_oneapi_fill_cmd_buffer (sycl::detail::ContextImplPtr Context, ur_exp_command_buffer_handle_t CommandBuffer, SYCLMemObjI *SYCLMemObj, void *Mem, size_t PatternSize, const unsigned char *Pattern, unsigned int Dim, sycl::range< 3 > Size, sycl::range< 3 > AccessRange, sycl::id< 3 > AccessOffset, unsigned int ElementSize, std::vector< ur_exp_command_buffer_sync_point_t > Deps, ur_exp_command_buffer_sync_point_t *OutSyncPoint)
 
static void ext_oneapi_prefetch_usm_cmd_buffer (sycl::detail::ContextImplPtr Context, ur_exp_command_buffer_handle_t CommandBuffer, void *Mem, size_t Length, std::vector< ur_exp_command_buffer_sync_point_t > Deps, ur_exp_command_buffer_sync_point_t *OutSyncPoint)
 
static void ext_oneapi_advise_usm_cmd_buffer (sycl::detail::ContextImplPtr Context, ur_exp_command_buffer_handle_t CommandBuffer, const void *Mem, size_t Length, ur_usm_advice_flags_t Advice, std::vector< ur_exp_command_buffer_sync_point_t > Deps, ur_exp_command_buffer_sync_point_t *OutSyncPoint)
 
static void copy_image_bindless (QueueImplPtr Queue, const void *Src, void *Dst, const ur_image_desc_t &SrcDesc, const ur_image_desc_t &DstDesc, const ur_image_format_t &SrcFormat, const ur_image_format_t &DstFormat, const ur_exp_image_copy_flags_t Flags, ur_rect_offset_t SrcOffset, ur_rect_offset_t DstOffset, ur_rect_region_t CopyExtent, const std::vector< ur_event_handle_t > &DepEvents, ur_event_handle_t *OutEvent)
 

Detailed Description

Definition at line 38 of file memory_manager.hpp.

Member Function Documentation

◆ advise_usm()

void sycl::_V1::detail::MemoryManager::advise_usm ( const void *  Ptr,
QueueImplPtr  Queue,
size_t  Len,
ur_usm_advice_flags_t  Advice,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 974 of file memory_manager.cpp.

Referenced by sycl::_V1::detail::queue_impl::mem_advise().

◆ allocate()

void * sycl::_V1::detail::MemoryManager::allocate ( ContextImplPtr  TargetContext,
SYCLMemObjI *  MemObj,
bool  InitFromUserData,
void *  HostPtr,
std::vector< EventImplPtr >  DepEvents,
ur_event_handle_t &  OutEvent 
)
static

Definition at line 281 of file memory_manager.cpp.

References sycl::_V1::detail::SYCLMemObjI::allocateMem(), and sycl::_V1::detail::waitForEvents().

◆ allocateBufferObject()

void * sycl::_V1::detail::MemoryManager::allocateBufferObject ( ContextImplPtr  TargetContext,
void *  UserPtr,
bool  HostPtrReadOnly,
const size_t  Size,
const sycl::property_list &  PropsList 
)
static

Definition at line 352 of file memory_manager.cpp.

References sycl::_V1::property_list::get_property(), sycl::_V1::detail::getMemObjCreationFlags(), sycl::_V1::property_list::has_property(), and sycl::_V1::detail::memBufferCreateHelper().

Referenced by allocateMemBuffer().

◆ allocateHostMemory()

void * sycl::_V1::detail::MemoryManager::allocateHostMemory ( SYCLMemObjI *  MemObj,
void *  UserPtr,
bool  HostPtrReadOnly,
size_t  Size,
const sycl::property_list &  PropsList 
)
static

Definition at line 294 of file memory_manager.cpp.

References sycl::_V1::detail::SYCLMemObjI::allocateHostMem().

Referenced by allocateMemBuffer(), and allocateMemImage().

◆ allocateImageObject()

void * sycl::_V1::detail::MemoryManager::allocateImageObject ( ContextImplPtr  TargetContext,
void *  UserPtr,
bool  HostPtrReadOnly,
const ur_image_desc_t &  Desc,
const ur_image_format_t &  Format,
const sycl::property_list &  PropsList 
)
static

Definition at line 336 of file memory_manager.cpp.

References sycl::_V1::detail::getMemObjCreationFlags().

Referenced by allocateMemImage().

◆ allocateInteropMemObject()

void * sycl::_V1::detail::MemoryManager::allocateInteropMemObject ( ContextImplPtr  TargetContext,
void *  UserPtr,
const EventImplPtr &  InteropEvent,
const ContextImplPtr &  InteropContext,
const sycl::property_list &  PropsList,
ur_event_handle_t &  OutEventToWait 
)
static

Definition at line 307 of file memory_manager.cpp.

Referenced by allocateMemBuffer(), and allocateMemImage().

◆ allocateMemBuffer()

void * sycl::_V1::detail::MemoryManager::allocateMemBuffer ( ContextImplPtr  TargetContext,
SYCLMemObjI *  MemObj,
void *  UserPtr,
bool  HostPtrReadOnly,
size_t  Size,
const EventImplPtr &  InteropEvent,
const ContextImplPtr &  InteropContext,
const sycl::property_list &  PropsList,
ur_event_handle_t &  OutEventToWait 
)
static

Definition at line 392 of file memory_manager.cpp.

References allocateBufferObject(), allocateHostMemory(), allocateInteropMemObject(), and sycl::_V1::detail::XPTIRegistry::bufferAssociateNotification().

Referenced by sycl::_V1::detail::buffer_impl::allocateMem().

◆ allocateMemImage()

void * sycl::_V1::detail::MemoryManager::allocateMemImage ( ContextImplPtr  TargetContext,
SYCLMemObjI *  MemObj,
void *  UserPtr,
bool  HostPtrReadOnly,
size_t  Size,
const ur_image_desc_t &  Desc,
const ur_image_format_t &  Format,
const EventImplPtr &  InteropEvent,
const ContextImplPtr &  InteropContext,
const sycl::property_list &  PropsList,
ur_event_handle_t &  OutEventToWait 
)
static

Definition at line 414 of file memory_manager.cpp.

References allocateHostMemory(), allocateImageObject(), and allocateInteropMemObject().

Referenced by sycl::_V1::detail::image_impl::allocateMem().

◆ allocateMemSubBuffer()

void * sycl::_V1::detail::MemoryManager::allocateMemSubBuffer ( ContextImplPtr  TargetContext,
void *  ParentMemObj,
size_t  ElemSize,
size_t  Offset,
range< 3 >  Range,
std::vector< EventImplPtr >  DepEvents,
ur_event_handle_t &  OutEvent 
)
static

Definition at line 430 of file memory_manager.cpp.

References sycl::_V1::invalid, sycl::_V1::make_error_code(), sycl::_V1::detail::set_ur_error(), and sycl::_V1::detail::waitForEvents().

◆ copy()

void sycl::_V1::detail::MemoryManager::copy ( SYCLMemObjI *  SYCLMemObj,
void *  SrcMem,
QueueImplPtr  SrcQueue,
unsigned int  DimSrc,
sycl::range< 3 >  SrcSize,
sycl::range< 3 >  SrcAccessRange,
sycl::id< 3 >  SrcOffset,
unsigned int  SrcElemSize,
void *  DstMem,
QueueImplPtr  TgtQueue,
unsigned int  DimDst,
sycl::range< 3 >  DstSize,
sycl::range< 3 >  DstAccessRange,
sycl::id< 3 >  DstOffset,
unsigned int  DstElemSize,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t &  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 759 of file memory_manager.cpp.

References sycl::_V1::detail::copyD2D(), sycl::_V1::detail::copyD2H(), sycl::_V1::detail::copyH2D(), and sycl::_V1::detail::copyH2H().

◆ copy_2d_usm()

void sycl::_V1::detail::MemoryManager::copy_2d_usm ( const void *  SrcMem,
size_t  SrcPitch,
QueueImplPtr  Queue,
void *  DstMem,
size_t  DstPitch,
size_t  Width,
size_t  Height,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 987 of file memory_manager.cpp.

◆ copy_from_device_global()

void sycl::_V1::detail::MemoryManager::copy_from_device_global ( const void *  DeviceGlobalPtr,
bool  IsDeviceImageScoped,
QueueImplPtr  Queue,
size_t  NumBytes,
size_t  Offset,
void *  DstMem,
const std::vector< ur_event_handle_t > &  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 1280 of file memory_manager.cpp.

References sycl::_V1::detail::DeviceGlobalMapEntry::MDeviceGlobalTSize, sycl::_V1::detail::memcpyFromDeviceGlobalDirect(), sycl::_V1::detail::memcpyFromDeviceGlobalUSM(), and sycl::_V1::detail::DeviceGlobalMapEntry::MIsDeviceImageScopeDecorated.

Referenced by sycl::_V1::detail::queue_impl::memcpyFromDeviceGlobal().

◆ copy_image_bindless()

void sycl::_V1::detail::MemoryManager::copy_image_bindless ( QueueImplPtr  Queue,
const void *  Src,
void *  Dst,
const ur_image_desc_t &  SrcDesc,
const ur_image_desc_t &  DstDesc,
const ur_image_format_t &  SrcFormat,
const ur_image_format_t &  DstFormat,
const ur_exp_image_copy_flags_t  Flags,
ur_rect_offset_t  SrcOffset,
ur_rect_offset_t  DstOffset,
ur_rect_region_t  CopyExtent,
const std::vector< ur_event_handle_t > &  DepEvents,
ur_event_handle_t *  OutEvent 
)
static

Definition at line 1616 of file memory_manager.cpp.

◆ copy_to_device_global()

void sycl::_V1::detail::MemoryManager::copy_to_device_global ( const void *  DeviceGlobalPtr,
bool  IsDeviceImageScoped,
QueueImplPtr  Queue,
size_t  NumBytes,
size_t  Offset,
const void *  SrcMem,
const std::vector< ur_event_handle_t > &  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 1258 of file memory_manager.cpp.

References sycl::_V1::detail::DeviceGlobalMapEntry::MDeviceGlobalTSize, sycl::_V1::detail::memcpyToDeviceGlobalDirect(), sycl::_V1::detail::memcpyToDeviceGlobalUSM(), and sycl::_V1::detail::DeviceGlobalMapEntry::MIsDeviceImageScopeDecorated.

Referenced by sycl::_V1::detail::queue_impl::memcpyToDeviceGlobal().

◆ copy_usm()

void sycl::_V1::detail::MemoryManager::copy_usm ( const void *  SrcMem,
QueueImplPtr  Queue,
size_t  Len,
void *  DstMem,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 907 of file memory_manager.cpp.

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

◆ ext_oneapi_advise_usm_cmd_buffer()

void sycl::_V1::detail::MemoryManager::ext_oneapi_advise_usm_cmd_buffer ( sycl::detail::ContextImplPtr  Context,
ur_exp_command_buffer_handle_t  CommandBuffer,
const void *  Mem,
size_t  Length,
ur_usm_advice_flags_t  Advice,
std::vector< ur_exp_command_buffer_sync_point_t >  Deps,
ur_exp_command_buffer_sync_point_t *  OutSyncPoint 
)
static

Definition at line 1605 of file memory_manager.cpp.

◆ ext_oneapi_copy_usm_cmd_buffer()

void sycl::_V1::detail::MemoryManager::ext_oneapi_copy_usm_cmd_buffer ( ContextImplPtr  Context,
const void *  SrcMem,
ur_exp_command_buffer_handle_t  CommandBuffer,
size_t  Len,
void *  DstMem,
std::vector< ur_exp_command_buffer_sync_point_t >  Deps,
ur_exp_command_buffer_sync_point_t *  OutSyncPoint 
)
static

Definition at line 1518 of file memory_manager.cpp.

◆ ext_oneapi_copyD2D_cmd_buffer()

void sycl::_V1::detail::MemoryManager::ext_oneapi_copyD2D_cmd_buffer ( sycl::detail::ContextImplPtr  Context,
ur_exp_command_buffer_handle_t  CommandBuffer,
SYCLMemObjI *  SYCLMemObj,
void *  SrcMem,
unsigned int  DimSrc,
sycl::range< 3 >  SrcSize,
sycl::range< 3 >  SrcAccessRange,
sycl::id< 3 >  SrcOffset,
unsigned int  SrcElemSize,
void *  DstMem,
unsigned int  DimDst,
sycl::range< 3 >  DstSize,
sycl::range< 3 >  DstAccessRange,
sycl::id< 3 >  DstOffset,
unsigned int  DstElemSize,
std::vector< ur_exp_command_buffer_sync_point_t >  Deps,
ur_exp_command_buffer_sync_point_t *  OutSyncPoint 
)
static

Definition at line 1303 of file memory_manager.cpp.

References sycl::_V1::detail::SYCLMemObjI::getType(), sycl::_V1::detail::prepTermPositions(), sycl::_V1::detail::TermPositions::XTerm, sycl::_V1::detail::TermPositions::YTerm, and sycl::_V1::detail::TermPositions::ZTerm.

◆ ext_oneapi_copyD2H_cmd_buffer()

void sycl::_V1::detail::MemoryManager::ext_oneapi_copyD2H_cmd_buffer ( sycl::detail::ContextImplPtr  Context,
ur_exp_command_buffer_handle_t  CommandBuffer,
SYCLMemObjI *  SYCLMemObj,
void *  SrcMem,
unsigned int  DimSrc,
sycl::range< 3 >  SrcSize,
sycl::range< 3 >  SrcAccessRange,
sycl::id< 3 >  SrcOffset,
unsigned int  SrcElemSize,
char *  DstMem,
unsigned int  DimDst,
sycl::range< 3 >  DstSize,
sycl::id< 3 >  DstOffset,
unsigned int  DstElemSize,
std::vector< ur_exp_command_buffer_sync_point_t >  Deps,
ur_exp_command_buffer_sync_point_t *  OutSyncPoint 
)
static

Definition at line 1369 of file memory_manager.cpp.

References sycl::_V1::detail::SYCLMemObjI::getType(), sycl::_V1::detail::prepTermPositions(), sycl::_V1::detail::TermPositions::XTerm, sycl::_V1::detail::TermPositions::YTerm, and sycl::_V1::detail::TermPositions::ZTerm.

◆ ext_oneapi_copyH2D_cmd_buffer()

void sycl::_V1::detail::MemoryManager::ext_oneapi_copyH2D_cmd_buffer ( sycl::detail::ContextImplPtr  Context,
ur_exp_command_buffer_handle_t  CommandBuffer,
SYCLMemObjI *  SYCLMemObj,
char *  SrcMem,
unsigned int  DimSrc,
sycl::range< 3 >  SrcSize,
sycl::id< 3 >  SrcOffset,
unsigned int  SrcElemSize,
void *  DstMem,
unsigned int  DimDst,
sycl::range< 3 >  DstSize,
sycl::range< 3 >  DstAccessRange,
sycl::id< 3 >  DstOffset,
unsigned int  DstElemSize,
std::vector< ur_exp_command_buffer_sync_point_t >  Deps,
ur_exp_command_buffer_sync_point_t *  OutSyncPoint 
)
static

Definition at line 1443 of file memory_manager.cpp.

References sycl::_V1::detail::SYCLMemObjI::getType(), sycl::_V1::detail::prepTermPositions(), sycl::_V1::detail::TermPositions::XTerm, sycl::_V1::detail::TermPositions::YTerm, and sycl::_V1::detail::TermPositions::ZTerm.

◆ ext_oneapi_fill_cmd_buffer()

void sycl::_V1::detail::MemoryManager::ext_oneapi_fill_cmd_buffer ( sycl::detail::ContextImplPtr  Context,
ur_exp_command_buffer_handle_t  CommandBuffer,
SYCLMemObjI *  SYCLMemObj,
void *  Mem,
size_t  PatternSize,
const unsigned char *  Pattern,
unsigned int  Dim,
sycl::range< 3 >  Size,
sycl::range< 3 >  AccessRange,
sycl::id< 3 >  AccessOffset,
unsigned int  ElementSize,
std::vector< ur_exp_command_buffer_sync_point_t >  Deps,
ur_exp_command_buffer_sync_point_t *  OutSyncPoint 
)
static

Definition at line 1557 of file memory_manager.cpp.

References sycl::_V1::detail::SYCLMemObjI::getType().

◆ ext_oneapi_fill_usm_cmd_buffer()

void sycl::_V1::detail::MemoryManager::ext_oneapi_fill_usm_cmd_buffer ( sycl::detail::ContextImplPtr  Context,
ur_exp_command_buffer_handle_t  CommandBuffer,
void *  DstMem,
size_t  Len,
const std::vector< unsigned char > &  Pattern,
std::vector< ur_exp_command_buffer_sync_point_t >  Deps,
ur_exp_command_buffer_sync_point_t *  OutSyncPoint 
)
static

Definition at line 1540 of file memory_manager.cpp.

◆ ext_oneapi_prefetch_usm_cmd_buffer()

void sycl::_V1::detail::MemoryManager::ext_oneapi_prefetch_usm_cmd_buffer ( sycl::detail::ContextImplPtr  Context,
ur_exp_command_buffer_handle_t  CommandBuffer,
void *  Mem,
size_t  Length,
std::vector< ur_exp_command_buffer_sync_point_t >  Deps,
ur_exp_command_buffer_sync_point_t *  OutSyncPoint 
)
static

Definition at line 1594 of file memory_manager.cpp.

◆ fill()

void sycl::_V1::detail::MemoryManager::fill ( SYCLMemObjI *  SYCLMemObj,
void *  Mem,
QueueImplPtr  Queue,
size_t  PatternSize,
const unsigned char *  Pattern,
unsigned int  Dim,
sycl::range< 3 >  Size,
sycl::range< 3 >  AccessRange,
sycl::id< 3 >  AccessOffset,
unsigned int  ElementSize,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t &  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 796 of file memory_manager.cpp.

References sycl::_V1::detail::SYCLMemObjI::getType().

◆ fill_2d_usm()

void sycl::_V1::detail::MemoryManager::fill_2d_usm ( void *  DstMem,
QueueImplPtr  Queue,
size_t  Pitch,
size_t  Width,
size_t  Height,
const std::vector< unsigned char > &  Pattern,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 1063 of file memory_manager.cpp.

◆ fill_usm()

void sycl::_V1::detail::MemoryManager::fill_usm ( void *  DstMem,
QueueImplPtr  Queue,
size_t  Len,
const std::vector< unsigned char > &  Pattern,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 935 of file memory_manager.cpp.

Referenced by sycl::_V1::detail::addCounterInit(), and sycl::_V1::detail::queue_impl::memset().

◆ map()

void * sycl::_V1::detail::MemoryManager::map ( SYCLMemObjI *  SYCLMemObj,
void *  Mem,
QueueImplPtr  Queue,
access::mode  AccessMode,
unsigned int  Dim,
sycl::range< 3 >  Size,
sycl::range< 3 >  AccessRange,
sycl::id< 3 >  AccessOffset,
unsigned int  ElementSize,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t &  OutEvent 
)
static

Definition at line 843 of file memory_manager.cpp.

References sycl::_V1::detail::memBufferMapHelper(), and sycl::_V1::detail::write().

◆ memset_2d_usm()

void sycl::_V1::detail::MemoryManager::memset_2d_usm ( void *  DstMem,
QueueImplPtr  Queue,
size_t  Pitch,
size_t  Width,
size_t  Height,
char  Value,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 1092 of file memory_manager.cpp.

◆ prefetch_usm()

void sycl::_V1::detail::MemoryManager::prefetch_usm ( void *  Ptr,
QueueImplPtr  Queue,
size_t  Len,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t *  OutEvent,
const detail::EventImplPtr &  OutEventImpl 
)
static

Definition at line 962 of file memory_manager.cpp.

◆ release()

void sycl::_V1::detail::MemoryManager::release ( ContextImplPtr  TargetContext,
SYCLMemObjI *  MemObj,
void *  MemAllocation,
std::vector< EventImplPtr >  DepEvents,
ur_event_handle_t &  OutEvent 
)
static

Definition at line 252 of file memory_manager.cpp.

References sycl::_V1::detail::XPTIRegistry::bufferReleaseNotification(), sycl::_V1::detail::SYCLMemObjI::releaseMem(), and sycl::_V1::detail::waitForEvents().

◆ releaseMemObj()

void sycl::_V1::detail::MemoryManager::releaseMemObj ( ContextImplPtr  TargetContext,
SYCLMemObjI *  MemObj,
void *  MemAllocation,
void *  UserPtr 
)
static

Definition at line 264 of file memory_manager.cpp.

References sycl::_V1::detail::memReleaseHelper(), and sycl::_V1::detail::SYCLMemObjI::releaseHostMem().

Referenced by sycl::_V1::detail::SYCLMemObjT::releaseMem().

◆ unmap()

void sycl::_V1::detail::MemoryManager::unmap ( SYCLMemObjI *  SYCLMemObj,
void *  Mem,
QueueImplPtr  Queue,
void *  MappedPtr,
std::vector< ur_event_handle_t >  DepEvents,
ur_event_handle_t &  OutEvent 
)
static

Definition at line 889 of file memory_manager.cpp.

References sycl::_V1::detail::memUnmapHelper().

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