SyclRuntimeWrappers.cpp File Reference

#include <level_zero/ze_api.h>
#include <sycl/ext/oneapi/backend/level_zero.hpp>
#include <sycl/sycl.hpp>

Go to the source code of this file.

Macros
#define	SYCL_RUNTIME_EXPORT
#define	L0_SAFE_CALL(call)

Functions
static sycl::device	getDefaultDevice ()
static sycl::context	getDefaultContext ()
static void *	allocDeviceMemory (sycl::queue *queue, size_t size, bool isShared)
static void	deallocDeviceMemory (sycl::queue *queue, void *ptr)
static ze_module_handle_t	loadModule (const void *data, size_t dataSize)
static sycl::kernel *	getKernel (ze_module_handle_t zeModule, const char *name)
static void	launchKernel (sycl::queue *queue, sycl::kernel *kernel, size_t gridX, size_t gridY, size_t gridZ, size_t blockX, size_t blockY, size_t blockZ, size_t sharedMemBytes, void **params, size_t paramsCount)
SYCL_RUNTIME_EXPORT sycl::queue *	mgpuStreamCreate ()
SYCL_RUNTIME_EXPORT void	mgpuStreamDestroy (sycl::queue *queue)
SYCL_RUNTIME_EXPORT void *	mgpuMemAlloc (uint64_t size, sycl::queue *queue, bool isShared)
SYCL_RUNTIME_EXPORT void	mgpuMemFree (void *ptr, sycl::queue *queue)
SYCL_RUNTIME_EXPORT ze_module_handle_t	mgpuModuleLoad (const void *data, size_t gpuBlobSize)
SYCL_RUNTIME_EXPORT sycl::kernel *	mgpuModuleGetFunction (ze_module_handle_t module, const char *name)
SYCL_RUNTIME_EXPORT void	mgpuLaunchKernel (sycl::kernel *kernel, size_t gridX, size_t gridY, size_t gridZ, size_t blockX, size_t blockY, size_t blockZ, size_t sharedMemBytes, sycl::queue *queue, void **params, void **, size_t paramsCount)
SYCL_RUNTIME_EXPORT void	mgpuStreamSynchronize (sycl::queue *queue)
SYCL_RUNTIME_EXPORT void	mgpuModuleUnload (ze_module_handle_t module)
SYCL_RUNTIME_EXPORT void	mgpuMemcpy (void *dst, void *src, size_t sizeBytes, sycl::queue *queue)

Macro Definition Documentation

L0_SAFE_CALL

#define L0_SAFE_CALL

(

call

)

Value:

  {                                                                            \
    ze_result_t status = (call);                                               \
    if (status != ZE_RESULT_SUCCESS) {                                         \
      fprintf(stdout, "L0 error %d\n", status);                                \
      fflush(stdout);                                                          \
      abort();                                                                 \
    }                                                                          \
  }

Definition at line 40 of file SyclRuntimeWrappers.cpp.

Referenced by getKernel(), loadModule(), and mgpuModuleUnload().

SYCL_RUNTIME_EXPORT

#define SYCL_RUNTIME_EXPORT

Definition at line 20 of file SyclRuntimeWrappers.cpp.

Referenced by mgpuMemFree(), mgpuStreamCreate(), mgpuStreamDestroy(), and mgpuStreamSynchronize().

Function Documentation

allocDeviceMemory()

void * allocDeviceMemory ( sycl::queue * queue, size_t size, bool isShared )

static

Definition at line 78 of file SyclRuntimeWrappers.cpp.

References getDefaultContext(), and getDefaultDevice().

Referenced by mgpuMemAlloc().

deallocDeviceMemory()

void deallocDeviceMemory ( sycl::queue * queue, void * ptr )

static

Definition at line 92 of file SyclRuntimeWrappers.cpp.

Referenced by mgpuMemFree().

getDefaultContext()

sycl::context getDefaultContext ( )

static

Definition at line 73 of file SyclRuntimeWrappers.cpp.

References getDefaultDevice().

Referenced by allocDeviceMemory(), getKernel(), loadModule(), and mgpuStreamCreate().

getDefaultDevice()

sycl::device getDefaultDevice ( )

static

Definition at line 52 of file SyclRuntimeWrappers.cpp.

Referenced by allocDeviceMemory(), getDefaultContext(), loadModule(), and mgpuStreamCreate().

getKernel()

sycl::kernel * getKernel ( ze_module_handle_t zeModule, const char * name )

static

Definition at line 114 of file SyclRuntimeWrappers.cpp.

References getDefaultContext(), and L0_SAFE_CALL.

Referenced by mgpuModuleGetFunction().

launchKernel()

void launchKernel ( sycl::queue * queue, sycl::kernel * kernel, size_t gridX, size_t gridY, size_t gridZ, size_t blockX, size_t blockY, size_t blockZ, size_t sharedMemBytes, void ** params, size_t paramsCount )

static

Definition at line 132 of file SyclRuntimeWrappers.cpp.

Referenced by mgpuLaunchKernel().

loadModule()

ze_module_handle_t loadModule ( const void * data, size_t dataSize )

static

Definition at line 96 of file SyclRuntimeWrappers.cpp.

References getDefaultContext(), getDefaultDevice(), and L0_SAFE_CALL.

Referenced by mgpuModuleLoad().

mgpuLaunchKernel()

SYCL_RUNTIME_EXPORT void mgpuLaunchKernel	(	sycl::kernel *	kernel,
		size_t	gridX,
		size_t	gridY,
		size_t	gridZ,
		size_t	blockX,
		size_t	blockY,
		size_t	blockZ,
		size_t	sharedMemBytes,
		sycl::queue *	queue,
		void **	params,
		void **	,
		size_t	paramsCount )

Definition at line 190 of file SyclRuntimeWrappers.cpp.

References launchKernel().

mgpuMemAlloc()

SYCL_RUNTIME_EXPORT void * mgpuMemAlloc	(	uint64_t	size,
		sycl::queue *	queue,
		bool	isShared )

Definition at line 165 of file SyclRuntimeWrappers.cpp.

References allocDeviceMemory().

mgpuMemcpy()

SYCL_RUNTIME_EXPORT void mgpuMemcpy	(	void *	dst,
		void *	src,
		size_t	sizeBytes,
		sycl::queue *	queue )

Definition at line 212 of file SyclRuntimeWrappers.cpp.

mgpuMemFree()

SYCL_RUNTIME_EXPORT void mgpuMemFree	(	void *	ptr,
		sycl::queue *	queue )

Definition at line 171 of file SyclRuntimeWrappers.cpp.

References deallocDeviceMemory(), and SYCL_RUNTIME_EXPORT.

mgpuModuleGetFunction()

SYCL_RUNTIME_EXPORT sycl::kernel * mgpuModuleGetFunction	(	ze_module_handle_t	module,
		const char *	name )

Definition at line 185 of file SyclRuntimeWrappers.cpp.

References getKernel().

mgpuModuleLoad()

SYCL_RUNTIME_EXPORT ze_module_handle_t mgpuModuleLoad	(	const void *	data,
		size_t	gpuBlobSize )

Definition at line 180 of file SyclRuntimeWrappers.cpp.

References loadModule().

mgpuModuleUnload()

SYCL_RUNTIME_EXPORT void mgpuModuleUnload

(

ze_module_handle_t

module

)

Definition at line 206 of file SyclRuntimeWrappers.cpp.

References L0_SAFE_CALL.

mgpuStreamCreate()

SYCL_RUNTIME_EXPORT sycl::queue * mgpuStreamCreate

(

)

Definition at line 151 of file SyclRuntimeWrappers.cpp.

References getDefaultContext(), getDefaultDevice(), and SYCL_RUNTIME_EXPORT.

mgpuStreamDestroy()

SYCL_RUNTIME_EXPORT void mgpuStreamDestroy

(

sycl::queue *

queue

)

Definition at line 160 of file SyclRuntimeWrappers.cpp.

References SYCL_RUNTIME_EXPORT.

mgpuStreamSynchronize()

SYCL_RUNTIME_EXPORT void mgpuStreamSynchronize

(

sycl::queue *

queue

)

Definition at line 200 of file SyclRuntimeWrappers.cpp.

References SYCL_RUNTIME_EXPORT.