77 static void *allocDeviceMemory(sycl::queue *queue, size_t size, bool isShared) {  in allocDeviceMemory()  argument
92 static void deallocDeviceMemory(sycl::queue *queue, void *ptr) {  in deallocDeviceMemory()  argument
93   sycl::free(ptr, *queue);  in deallocDeviceMemory()
132 static void launchKernel(sycl::queue *queue, sycl::kernel *kernel, size_t gridX,  in launchKernel()  argument
141   queue->submit([&](sycl::handler &cgh) {  in launchKernel()
151 extern "C" SYCL_RUNTIME_EXPORT sycl::queue *mgpuStreamCreate() {  in mgpuStreamCreate()
154     sycl::queue *queue =  in mgpuStreamCreate()  local
155         new sycl::queue(getDefaultContext(), getDefaultDevice());  in mgpuStreamCreate()
156     return queue;  in mgpuStreamCreate()
160 extern "C" SYCL_RUNTIME_EXPORT void mgpuStreamDestroy(sycl::queue *queue) {  in mgpuStreamDestroy()  argument
161   catchAll([&]() { delete queue; });  in mgpuStreamDestroy()
165 mgpuMemAlloc(uint64_t size, sycl::queue *queue, bool isShared) {  in mgpuMemAlloc()  argument
167     return allocDeviceMemory(queue, static_cast<size_t>(size), true);  in mgpuMemAlloc()
171 extern "C" SYCL_RUNTIME_EXPORT void mgpuMemFree(void *ptr, sycl::queue *queue) {  in mgpuMemFree()  argument
174       deallocDeviceMemory(queue, ptr);  in mgpuMemFree()
192                  size_t sharedMemBytes, sycl::queue *queue, void **params,  in mgpuLaunchKernel()  argument
195     launchKernel(queue, kernel, gridX, gridY, gridZ, blockX, blockY, blockZ,  in mgpuLaunchKernel()
200 extern "C" SYCL_RUNTIME_EXPORT void mgpuStreamSynchronize(sycl::queue *queue) {  in mgpuStreamSynchronize()  argument
202   catchAll([&]() { queue->wait(); });  in mgpuStreamSynchronize()