Skip to content
New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

Sign up for GitHub

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Jump to bottom

[SYCL][Bindless][Doc][ABI-Break] Rename external semaphore destroy to release #14535

Merged
merged 8 commits into from
Jul 18, 2024
Merged

[SYCL][Bindless][Doc][ABI-Break] Rename external semaphore destroy to release #14535

Show file tree
Hide file tree
Changes from all commits
Commits
Show all changes
8 commits
Select commit Hold shift + click to select a range
4c9d4d8
[SYCL][Bindless][Doc][ABI-Break] Rename external semaphore destroy to…
Seanst98 Jul 10, 2024
5eb867f
Address feedback on spec wording
Seanst98 Jul 11, 2024
264a12f
Address feedback on spec wording
Seanst98 Jul 11, 2024
f54e415
Merge branch 'sycl' into sean/rename-external-semaphore-release
Seanst98 Jul 12, 2024
d71a57f
Merge branch 'sycl' into sean/rename-external-semaphore-release
Seanst98 Jul 17, 2024
927610b
Merge branch 'sycl' into sean/rename-external-semaphore-release
Seanst98 Jul 17, 2024
8958978
Merge branch 'sycl' into sean/rename-external-semaphore-release
Seanst98 Jul 18, 2024
2dfdc06
Update UR CMakeLists
Seanst98 Jul 18, 2024
File filter

Filter by extension

Filter by extension
Conversations
Failed to load comments.
Loading
Jump to
Jump to file
Failed to load files.
Loading
Diff view
Diff view
15 changes: 9 additions & 6 deletions sycl/doc/extensions/experimental/sycl_ext_oneapi_bindless_images.asciidoc
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -1903,17 +1903,18 @@ the `ext_oneapi_signal_external_semaphore` call complete.
`ext_oneapi_wait_external_semaphore` and `ext_oneapi_signal_external_semaphore`
are non-blocking, asynchronous operations.

The user must ensure to destroy all external semaphore objects once they are no
longer required through `destroy_external_semaphore`.
The user must ensure to destroy all SYCL external semaphore objects used to
access the external semaphore once they are no longer required through
`release_external_semaphore`.

```cpp
namespace sycl::ext::oneapi::experimental {

void destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
void release_external_semaphore(interop_semaphore_handle semaphoreHandle,
const sycl::device &syclDevice,
const sycl::context &syclContext);

void destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
void release_external_semaphore(interop_semaphore_handle semaphoreHandle,
const sycl::queue &syclQueue);

}
Expand Down Expand Up @@ -2579,9 +2580,9 @@ try {
input_interop_mem_handle, queue);
sycl::ext::oneapi::experimental::release_external_memory(
output_interop_mem_handle, queue);
sycl::ext::oneapi::experimental::destroy_external_semaphore(
sycl::ext::oneapi::experimental::release_external_semaphore(
wait_interop_semaphore_handle, queue);
sycl::ext::oneapi::experimental::destroy_external_semaphore(
sycl::ext::oneapi::experimental::release_external_semaphore(
done_interop_semaphore_handle, queue);
sycl::ext::oneapi::experimental::destroy_image_handle(img_input, queue);
sycl::ext::oneapi::experimental::destroy_image_handle(img_output, queue);
Expand Down Expand Up @@ -2808,4 +2809,6 @@ These features still need to be handled:
- Fetch sampled image arrays with `fetch_image_array` API.
|5.13|2024-07-10| - Added const-qualifiers to `Src` param in `ext_oneapi_copy`
funcs.
|5.14|2024-07-17| - Rename `destroy_external_semaphore` to
`release_external_semaphore`.
|======================
2 changes: 1 addition & 1 deletion sycl/include/sycl/detail/pi.def
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -209,7 +209,7 @@ _PI_API(piextImportExternalMemory)
_PI_API(piextMemReleaseInterop)
_PI_API(piextMemMapExternalArray)
_PI_API(piextImportExternalSemaphore)
_PI_API(piextDestroyExternalSemaphore)
_PI_API(piextReleaseExternalSemaphore)
_PI_API(piextWaitExternalSemaphore)
_PI_API(piextSignalExternalSemaphore)

Expand Down
9 changes: 5 additions & 4 deletions sycl/include/sycl/detail/pi.h
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -203,9 +203,10 @@
// 17.59 Added const-qualifier to src_ptr in piextMemImageCopy.
// 18.60 Remove deprecated functions piextMemImportOpaqueFD and
// piextImportExternalSemaphoreOpaqueFD
// 19.61 Rename piextDestroyExternalSemaphore to piextReleaseExternalSemaphore

#define _PI_H_VERSION_MAJOR 18
#define _PI_H_VERSION_MINOR 60
#define _PI_H_VERSION_MAJOR 19
#define _PI_H_VERSION_MINOR 61

#define _PI_STRING_HELPER(a) #a
#define _PI_CONCAT(a, b) _PI_STRING_HELPER(a.b)
Expand Down Expand Up @@ -3163,14 +3164,14 @@ piextImportExternalSemaphore(pi_context context, pi_device device,
pi_external_semaphore_descriptor *sem_descriptor,
pi_interop_semaphore_handle *ret_handle);

/// API to destroy the external semaphore handle.
/// API to release the external semaphore.
///
/// \param context is the pi_context
/// \param device is the pi_device
/// \param sem_handle is the interop semaphore handle to the external semaphore
/// to be destroyed
__SYCL_EXPORT pi_result
piextDestroyExternalSemaphore(pi_context context, pi_device device,
piextReleaseExternalSemaphore(pi_context context, pi_device device,
pi_interop_semaphore_handle sem_handle);

/// API to instruct the queue with a non-blocking wait on an external semaphore.
Expand Down
8 changes: 4 additions & 4 deletions sycl/include/sycl/ext/oneapi/bindless_images.hpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -224,7 +224,7 @@ __SYCL_EXPORT interop_semaphore_handle import_external_semaphore(
const sycl::queue &syclQueue);

/**
* @brief Destroy the external semaphore handle
* @brief Release the external semaphore
*
* @param semaphoreHandle The interop semaphore handle to destroy
* @param syclDevice The device in which the interop semaphore handle was
Expand All @@ -233,19 +233,19 @@ __SYCL_EXPORT interop_semaphore_handle import_external_semaphore(
* created
*/
__SYCL_EXPORT void
destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
release_external_semaphore(interop_semaphore_handle semaphoreHandle,
const sycl::device &syclDevice,
const sycl::context &syclContext);

/**
* @brief Destroy the external semaphore handle
* @brief Release the external semaphore
*
* @param semaphoreHandle The interop semaphore handle to destroy
* @param syclQueue The queue in which the interop semaphore handle was
* created
*/
__SYCL_EXPORT void
destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
release_external_semaphore(interop_semaphore_handle semaphoreHandle,
const sycl::queue &syclQueue);

/**
Expand Down
4 changes: 2 additions & 2 deletions sycl/plugins/cuda/pi_cuda.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -484,9 +484,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
}

__SYCL_EXPORT pi_result
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
pi_interop_semaphore_handle SemHandle) {
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
}

__SYCL_EXPORT pi_result piextWaitExternalSemaphore(
Expand Down
4 changes: 2 additions & 2 deletions sycl/plugins/hip/pi_hip.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -487,9 +487,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
}

__SYCL_EXPORT pi_result
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
pi_interop_semaphore_handle SemHandle) {
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
}

__SYCL_EXPORT pi_result piextWaitExternalSemaphore(
Expand Down
4 changes: 2 additions & 2 deletions sycl/plugins/level_zero/pi_level_zero.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -496,9 +496,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
}

__SYCL_EXPORT pi_result
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
pi_interop_semaphore_handle SemHandle) {
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
}

__SYCL_EXPORT pi_result piextWaitExternalSemaphore(
Expand Down
4 changes: 2 additions & 2 deletions sycl/plugins/native_cpu/pi_native_cpu.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -491,9 +491,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
}

__SYCL_EXPORT pi_result
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
pi_interop_semaphore_handle SemHandle) {
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
}

__SYCL_EXPORT pi_result piextWaitExternalSemaphore(
Expand Down
4 changes: 2 additions & 2 deletions sycl/plugins/opencl/pi_opencl.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -467,9 +467,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
RetHandle);
}

pi_result piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
pi_result piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
pi_interop_semaphore_handle SemHandle) {
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
}

__SYCL_EXPORT pi_result piextWaitExternalSemaphore(
Expand Down
10 changes: 5 additions & 5 deletions sycl/plugins/unified_runtime/CMakeLists.txt
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -100,12 +100,12 @@ if(SYCL_PI_UR_USE_FETCH_CONTENT)
endfunction()

set(UNIFIED_RUNTIME_REPO "https://github.com/oneapi-src/unified-runtime.git")
# commit 6c2329edef40cdacb8e28704eb02172c4c17a903
# commit 0abf37072567c27ff412ea7acfce7b72b9e4b3c0
# Author: Kenneth Benzie (Benie) <k.benzie@codeplay.com>
# Date: Tue Jul 16 21:04:25 2024 +0100
# Merge pull request #1743 from Seanst98/sean/copy-const-qualifiers
# [Bindless][Exp] Add const-qualifier to Src param in urBindlessImagesImageCopyExp
set(UNIFIED_RUNTIME_TAG 6c2329edef40cdacb8e28704eb02172c4c17a903)
# Date: Wed Jul 17 19:12:31 2024 +0100
# Reinstate "Merge pull request #1855 from Seanst98/sean/rename-external-semaphore-release""
# This reverts commit b26e53cdbd178ee03c3e8252aa00e596deb1f313.
set(UNIFIED_RUNTIME_TAG 0abf37072567c27ff412ea7acfce7b72b9e4b3c0)

fetch_adapter_source(level_zero
${UNIFIED_RUNTIME_REPO}
Expand Down
4 changes: 2 additions & 2 deletions sycl/plugins/unified_runtime/pi2ur.hpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -5618,7 +5618,7 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
}

inline pi_result
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
pi_interop_semaphore_handle SemHandle) {
PI_ASSERT(Context, PI_ERROR_INVALID_CONTEXT);
PI_ASSERT(Device, PI_ERROR_INVALID_DEVICE);
Expand All @@ -5628,7 +5628,7 @@ piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
auto UrSemHandle =
reinterpret_cast<ur_exp_interop_semaphore_handle_t>(SemHandle);

HANDLE_ERRORS(urBindlessImagesDestroyExternalSemaphoreExp(UrContext, UrDevice,
HANDLE_ERRORS(urBindlessImagesReleaseExternalSemaphoreExp(UrContext, UrDevice,
UrSemHandle));

return PI_SUCCESS;
Expand Down
4 changes: 2 additions & 2 deletions sycl/plugins/unified_runtime/pi_unified_runtime.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -1419,9 +1419,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
}

__SYCL_EXPORT pi_result
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
pi_interop_semaphore_handle SemHandle) {
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
}

__SYCL_EXPORT pi_result piextWaitExternalSemaphore(
Expand Down
8 changes: 4 additions & 4 deletions sycl/source/detail/bindless_images.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -620,7 +620,7 @@ __SYCL_EXPORT interop_semaphore_handle import_external_semaphore(
}

__SYCL_EXPORT void
destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
release_external_semaphore(interop_semaphore_handle semaphoreHandle,
const sycl::device &syclDevice,
const sycl::context &syclContext) {
std::shared_ptr<sycl::detail::context_impl> CtxImpl =
Expand All @@ -632,14 +632,14 @@ destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
pi_device Device = DevImpl->getHandleRef();

Plugin->call<sycl::errc::invalid,
sycl::detail::PiApiKind::piextDestroyExternalSemaphore>(
sycl::detail::PiApiKind::piextReleaseExternalSemaphore>(
C, Device, (pi_interop_semaphore_handle)semaphoreHandle.raw_handle);
}

__SYCL_EXPORT void
destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
release_external_semaphore(interop_semaphore_handle semaphoreHandle,
const sycl::queue &syclQueue) {
destroy_external_semaphore(semaphoreHandle, syclQueue.get_device(),
release_external_semaphore(semaphoreHandle, syclQueue.get_device(),
syclQueue.get_context());
}

Expand Down
4 changes: 2 additions & 2 deletions sycl/test-e2e/bindless_images/vulkan_interop/unsampled_images.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -134,9 +134,9 @@ create_test_handles(sycl::context &ctxt, sycl::device &dev,
}

void cleanup_test(sycl::context &ctxt, sycl::device &dev, handles_t handles) {
syclexp::destroy_external_semaphore(
syclexp::release_external_semaphore(
handles.sycl_wait_interop_semaphore_handle, dev, ctxt);
syclexp::destroy_external_semaphore(
syclexp::release_external_semaphore(
handles.sycl_done_interop_semaphore_handle, dev, ctxt);
syclexp::destroy_image_handle(handles.input_1, dev, ctxt);
syclexp::destroy_image_handle(handles.input_2, dev, ctxt);
Expand Down
4 changes: 2 additions & 2 deletions sycl/test/abi/pi_cuda_symbol_check.dump
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -106,14 +106,14 @@ piextCommandBufferUpdateKernelLaunch
piextContextCreateWithNativeHandle
piextContextGetNativeHandle
piextContextSetExtendedDeleter
piextDestroyExternalSemaphore
piextDeviceCreateWithNativeHandle
piextDeviceGetNativeHandle
piextDeviceSelectBinary
piextDisablePeerAccess
piextEnablePeerAccess
piextEnqueueCommandBuffer
piextEnqueueCooperativeKernelLaunch
piextEnqueueKernelLaunchCustom
piextEnqueueNativeCommand
piextEnqueueReadHostPipe
piextEnqueueWriteHostPipe
Expand Down Expand Up @@ -157,6 +157,7 @@ piextProgramSetSpecializationConstant
piextQueueCreate
piextQueueCreateWithNativeHandle
piextQueueGetNativeHandle
piextReleaseExternalSemaphore
piextSignalExternalSemaphore
piextUSMDeviceAlloc
piextUSMEnqueueFill
Expand All @@ -181,4 +182,3 @@ piextVirtualMemReserve
piextVirtualMemSetAccess
piextVirtualMemUnmap
piextWaitExternalSemaphore
piextEnqueueKernelLaunchCustom
2 changes: 1 addition & 1 deletion sycl/test/abi/pi_hip_symbol_check.dump
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -106,7 +106,7 @@ piextCommandBufferUpdateKernelLaunch
piextContextCreateWithNativeHandle
piextContextGetNativeHandle
piextContextSetExtendedDeleter
piextDestroyExternalSemaphore
piextReleaseExternalSemaphore
piextDeviceCreateWithNativeHandle
piextDeviceGetNativeHandle
piextDeviceSelectBinary
Expand Down
4 changes: 2 additions & 2 deletions sycl/test/abi/pi_level_zero_symbol_check.dump
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -105,14 +105,14 @@ piextCommandBufferUpdateKernelLaunch
piextContextCreateWithNativeHandle
piextContextGetNativeHandle
piextContextSetExtendedDeleter
piextDestroyExternalSemaphore
piextDeviceCreateWithNativeHandle
piextDeviceGetNativeHandle
piextDeviceSelectBinary
piextDisablePeerAccess
piextEnablePeerAccess
piextEnqueueCommandBuffer
piextEnqueueCooperativeKernelLaunch
piextEnqueueKernelLaunchCustom
piextEnqueueNativeCommand
piextEnqueueReadHostPipe
piextEnqueueWriteHostPipe
Expand Down Expand Up @@ -156,6 +156,7 @@ piextProgramSetSpecializationConstant
piextQueueCreate
piextQueueCreateWithNativeHandle
piextQueueGetNativeHandle
piextReleaseExternalSemaphore
piextSignalExternalSemaphore
piextUSMDeviceAlloc
piextUSMEnqueueFill
Expand All @@ -180,4 +181,3 @@ piextVirtualMemReserve
piextVirtualMemSetAccess
piextVirtualMemUnmap
piextWaitExternalSemaphore
piextEnqueueKernelLaunchCustom
2 changes: 1 addition & 1 deletion sycl/test/abi/pi_nativecpu_symbol_check.dump
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -106,7 +106,7 @@ piextCommandBufferUpdateKernelLaunch
piextContextCreateWithNativeHandle
piextContextGetNativeHandle
piextContextSetExtendedDeleter
piextDestroyExternalSemaphore
piextReleaseExternalSemaphore
piextDeviceCreateWithNativeHandle
piextDeviceGetNativeHandle
piextDeviceSelectBinary
Expand Down
10 changes: 5 additions & 5 deletions sycl/test/abi/pi_opencl_symbol_check.dump
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -105,14 +105,14 @@ piextCommandBufferUpdateKernelLaunch
piextContextCreateWithNativeHandle
piextContextGetNativeHandle
piextContextSetExtendedDeleter
piextDestroyExternalSemaphore
piextDeviceCreateWithNativeHandle
piextDeviceGetNativeHandle
piextDeviceSelectBinary
piextDisablePeerAccess
piextEnablePeerAccess
piextEnqueueCommandBuffer
piextEnqueueCooperativeKernelLaunch
piextEnqueueKernelLaunchCustom
piextEnqueueNativeCommand
piextEnqueueReadHostPipe
piextEnqueueWriteHostPipe
Expand All @@ -133,9 +133,6 @@ piextMemGetNativeHandle
piextMemImageAllocate
piextMemImageCopy
piextMemImageCreateWithNativeHandle
piextPhysicalMemCreate
piextPhysicalMemRelease
piextPhysicalMemRetain
piextMemImageFree
piextMemImageGetInfo
piextMemMapExternalArray
Expand All @@ -147,6 +144,9 @@ piextMemSampledImageHandleDestroy
piextMemUnsampledImageCreate
piextMemUnsampledImageHandleDestroy
piextPeerAccessGetInfo
piextPhysicalMemCreate
piextPhysicalMemRelease
piextPhysicalMemRetain
piextPlatformCreateWithNativeHandle
piextPlatformGetNativeHandle
piextPluginGetOpaqueData
Expand All @@ -156,6 +156,7 @@ piextProgramSetSpecializationConstant
piextQueueCreate
piextQueueCreateWithNativeHandle
piextQueueGetNativeHandle
piextReleaseExternalSemaphore
piextSignalExternalSemaphore
piextUSMDeviceAlloc
piextUSMEnqueueFill
Expand All @@ -180,4 +181,3 @@ piextVirtualMemReserve
piextVirtualMemSetAccess
piextVirtualMemUnmap
piextWaitExternalSemaphore
piextEnqueueKernelLaunchCustom
4 changes: 2 additions & 2 deletions sycl/test/abi/sycl_symbols_linux.dump
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -3045,8 +3045,8 @@ _ZN4sycl3_V13ext6oneapi12experimental25import_external_semaphoreINS3_21resource_
_ZN4sycl3_V13ext6oneapi12experimental25import_external_semaphoreINS3_21resource_win32_handleEEENS3_24interop_semaphore_handleENS3_29external_semaphore_descriptorIT_EERKNS0_6deviceERKNS0_7contextE
_ZN4sycl3_V13ext6oneapi12experimental25map_external_image_memoryENS3_18interop_mem_handleERKNS3_16image_descriptorERKNS0_5queueE
_ZN4sycl3_V13ext6oneapi12experimental25map_external_image_memoryENS3_18interop_mem_handleERKNS3_16image_descriptorERKNS0_6deviceERKNS0_7contextE
_ZN4sycl3_V13ext6oneapi12experimental26destroy_external_semaphoreENS3_24interop_semaphore_handleERKNS0_5queueE
_ZN4sycl3_V13ext6oneapi12experimental26destroy_external_semaphoreENS3_24interop_semaphore_handleERKNS0_6deviceERKNS0_7contextE
_ZN4sycl3_V13ext6oneapi12experimental26release_external_semaphoreENS3_24interop_semaphore_handleERKNS0_5queueE
_ZN4sycl3_V13ext6oneapi12experimental26release_external_semaphoreENS3_24interop_semaphore_handleERKNS0_6deviceERKNS0_7contextE
_ZN4sycl3_V13ext6oneapi12experimental4node12update_rangeILi1EEEvNS0_5rangeIXT_EEE
_ZN4sycl3_V13ext6oneapi12experimental4node12update_rangeILi2EEEvNS0_5rangeIXT_EEE
_ZN4sycl3_V13ext6oneapi12experimental4node12update_rangeILi3EEEvNS0_5rangeIXT_EEE
Expand Down
Loading
Loading