Skip to content

Commit 13c9d0e

Browse files
Seanst98Seanst98
authored
[SYCL][Bindless][Doc][ABI-Break] Rename external semaphore destroy to release (#14535)
Rename function destroy_external_semaphore to release_external_semaphore. This name change is to clarify exactly what is happening to the external semaphore. That is, it is being released not destroyed. Corresponding UR PR: oneapi-src/unified-runtime#1855
1 parent 5647f9f commit 13c9d0e

File tree

22 files changed

+60
-56
lines changed

22 files changed

+60
-56
lines changed

‎sycl/doc/extensions/experimental/sycl_ext_oneapi_bindless_images.asciidoc

Lines changed: 9 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -1903,17 +1903,18 @@ the `ext_oneapi_signal_external_semaphore` call complete.
19031903
`ext_oneapi_wait_external_semaphore` and `ext_oneapi_signal_external_semaphore`
19041904
are non-blocking, asynchronous operations.
19051905

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

19091910
```cpp
19101911
namespace sycl::ext::oneapi::experimental {
19111912

1912-
void destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
1913+
void release_external_semaphore(interop_semaphore_handle semaphoreHandle,
19131914
const sycl::device &syclDevice,
19141915
const sycl::context &syclContext);
19151916

1916-
void destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
1917+
void release_external_semaphore(interop_semaphore_handle semaphoreHandle,
19171918
const sycl::queue &syclQueue);
19181919

19191920
}
@@ -2579,9 +2580,9 @@ try {
25792580
input_interop_mem_handle, queue);
25802581
sycl::ext::oneapi::experimental::release_external_memory(
25812582
output_interop_mem_handle, queue);
2582-
sycl::ext::oneapi::experimental::destroy_external_semaphore(
2583+
sycl::ext::oneapi::experimental::release_external_semaphore(
25832584
wait_interop_semaphore_handle, queue);
2584-
sycl::ext::oneapi::experimental::destroy_external_semaphore(
2585+
sycl::ext::oneapi::experimental::release_external_semaphore(
25852586
done_interop_semaphore_handle, queue);
25862587
sycl::ext::oneapi::experimental::destroy_image_handle(img_input, queue);
25872588
sycl::ext::oneapi::experimental::destroy_image_handle(img_output, queue);
@@ -2808,4 +2809,6 @@ These features still need to be handled:
28082809
- Fetch sampled image arrays with `fetch_image_array` API.
28092810
|5.13|2024-07-10| - Added const-qualifiers to `Src` param in `ext_oneapi_copy`
28102811
funcs.
2812+
|5.14|2024-07-17| - Rename `destroy_external_semaphore` to
2813+
`release_external_semaphore`.
28112814
|======================

‎sycl/include/sycl/detail/pi.def

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -209,7 +209,7 @@ _PI_API(piextImportExternalMemory)
209209
_PI_API(piextMemReleaseInterop)
210210
_PI_API(piextMemMapExternalArray)
211211
_PI_API(piextImportExternalSemaphore)
212-
_PI_API(piextDestroyExternalSemaphore)
212+
_PI_API(piextReleaseExternalSemaphore)
213213
_PI_API(piextWaitExternalSemaphore)
214214
_PI_API(piextSignalExternalSemaphore)
215215

‎sycl/include/sycl/detail/pi.h

Lines changed: 5 additions & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -203,9 +203,10 @@
203203
// 17.59 Added const-qualifier to src_ptr in piextMemImageCopy.
204204
// 18.60 Remove deprecated functions piextMemImportOpaqueFD and
205205
// piextImportExternalSemaphoreOpaqueFD
206+
// 19.61 Rename piextDestroyExternalSemaphore to piextReleaseExternalSemaphore
206207

207-
#define _PI_H_VERSION_MAJOR 18
208-
#define _PI_H_VERSION_MINOR 60
208+
#define _PI_H_VERSION_MAJOR 19
209+
#define _PI_H_VERSION_MINOR 61
209210

210211
#define _PI_STRING_HELPER(a) #a
211212
#define _PI_CONCAT(a, b) _PI_STRING_HELPER(a.b)
@@ -3163,14 +3164,14 @@ piextImportExternalSemaphore(pi_context context, pi_device device,
31633164
pi_external_semaphore_descriptor *sem_descriptor,
31643165
pi_interop_semaphore_handle *ret_handle);
31653166

3166-
/// API to destroy the external semaphore handle.
3167+
/// API to release the external semaphore.
31673168
///
31683169
/// \param context is the pi_context
31693170
/// \param device is the pi_device
31703171
/// \param sem_handle is the interop semaphore handle to the external semaphore
31713172
/// to be destroyed
31723173
__SYCL_EXPORT pi_result
3173-
piextDestroyExternalSemaphore(pi_context context, pi_device device,
3174+
piextReleaseExternalSemaphore(pi_context context, pi_device device,
31743175
pi_interop_semaphore_handle sem_handle);
31753176

31763177
/// API to instruct the queue with a non-blocking wait on an external semaphore.

‎sycl/include/sycl/ext/oneapi/bindless_images.hpp

Lines changed: 4 additions & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -224,7 +224,7 @@ __SYCL_EXPORT interop_semaphore_handle import_external_semaphore(
224224
const sycl::queue &syclQueue);
225225

226226
/**
227-
* @brief Destroy the external semaphore handle
227+
* @brief Release the external semaphore
228228
*
229229
* @param semaphoreHandle The interop semaphore handle to destroy
230230
* @param syclDevice The device in which the interop semaphore handle was
@@ -233,19 +233,19 @@ __SYCL_EXPORT interop_semaphore_handle import_external_semaphore(
233233
* created
234234
*/
235235
__SYCL_EXPORT void
236-
destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
236+
release_external_semaphore(interop_semaphore_handle semaphoreHandle,
237237
const sycl::device &syclDevice,
238238
const sycl::context &syclContext);
239239

240240
/**
241-
* @brief Destroy the external semaphore handle
241+
* @brief Release the external semaphore
242242
*
243243
* @param semaphoreHandle The interop semaphore handle to destroy
244244
* @param syclQueue The queue in which the interop semaphore handle was
245245
* created
246246
*/
247247
__SYCL_EXPORT void
248-
destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
248+
release_external_semaphore(interop_semaphore_handle semaphoreHandle,
249249
const sycl::queue &syclQueue);
250250

251251
/**

‎sycl/plugins/cuda/pi_cuda.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -484,9 +484,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
484484
}
485485

486486
__SYCL_EXPORT pi_result
487-
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
487+
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
488488
pi_interop_semaphore_handle SemHandle) {
489-
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
489+
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
490490
}
491491

492492
__SYCL_EXPORT pi_result piextWaitExternalSemaphore(

‎sycl/plugins/hip/pi_hip.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -487,9 +487,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
487487
}
488488

489489
__SYCL_EXPORT pi_result
490-
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
490+
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
491491
pi_interop_semaphore_handle SemHandle) {
492-
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
492+
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
493493
}
494494

495495
__SYCL_EXPORT pi_result piextWaitExternalSemaphore(

‎sycl/plugins/level_zero/pi_level_zero.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -496,9 +496,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
496496
}
497497

498498
__SYCL_EXPORT pi_result
499-
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
499+
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
500500
pi_interop_semaphore_handle SemHandle) {
501-
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
501+
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
502502
}
503503

504504
__SYCL_EXPORT pi_result piextWaitExternalSemaphore(

‎sycl/plugins/native_cpu/pi_native_cpu.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -491,9 +491,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
491491
}
492492

493493
__SYCL_EXPORT pi_result
494-
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
494+
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
495495
pi_interop_semaphore_handle SemHandle) {
496-
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
496+
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
497497
}
498498

499499
__SYCL_EXPORT pi_result piextWaitExternalSemaphore(

‎sycl/plugins/opencl/pi_opencl.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -467,9 +467,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
467467
RetHandle);
468468
}
469469

470-
pi_result piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
470+
pi_result piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
471471
pi_interop_semaphore_handle SemHandle) {
472-
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
472+
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
473473
}
474474

475475
__SYCL_EXPORT pi_result piextWaitExternalSemaphore(

‎sycl/plugins/unified_runtime/CMakeLists.txt

Lines changed: 5 additions & 5 deletions
Original file line numberDiff line numberDiff line change
@@ -100,12 +100,12 @@ if(SYCL_PI_UR_USE_FETCH_CONTENT)
100100
endfunction()
101101

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

110110
fetch_adapter_source(level_zero
111111
${UNIFIED_RUNTIME_REPO}

‎sycl/plugins/unified_runtime/pi2ur.hpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -5618,7 +5618,7 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
56185618
}
56195619

56205620
inline pi_result
5621-
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
5621+
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
56225622
pi_interop_semaphore_handle SemHandle) {
56235623
PI_ASSERT(Context, PI_ERROR_INVALID_CONTEXT);
56245624
PI_ASSERT(Device, PI_ERROR_INVALID_DEVICE);
@@ -5628,7 +5628,7 @@ piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
56285628
auto UrSemHandle =
56295629
reinterpret_cast<ur_exp_interop_semaphore_handle_t>(SemHandle);
56305630

5631-
HANDLE_ERRORS(urBindlessImagesDestroyExternalSemaphoreExp(UrContext, UrDevice,
5631+
HANDLE_ERRORS(urBindlessImagesReleaseExternalSemaphoreExp(UrContext, UrDevice,
56325632
UrSemHandle));
56335633

56345634
return PI_SUCCESS;

‎sycl/plugins/unified_runtime/pi_unified_runtime.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -1419,9 +1419,9 @@ piextImportExternalSemaphore(pi_context Context, pi_device Device,
14191419
}
14201420

14211421
__SYCL_EXPORT pi_result
1422-
piextDestroyExternalSemaphore(pi_context Context, pi_device Device,
1422+
piextReleaseExternalSemaphore(pi_context Context, pi_device Device,
14231423
pi_interop_semaphore_handle SemHandle) {
1424-
return pi2ur::piextDestroyExternalSemaphore(Context, Device, SemHandle);
1424+
return pi2ur::piextReleaseExternalSemaphore(Context, Device, SemHandle);
14251425
}
14261426

14271427
__SYCL_EXPORT pi_result piextWaitExternalSemaphore(

‎sycl/source/detail/bindless_images.cpp

Lines changed: 4 additions & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -620,7 +620,7 @@ __SYCL_EXPORT interop_semaphore_handle import_external_semaphore(
620620
}
621621

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

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

639639
__SYCL_EXPORT void
640-
destroy_external_semaphore(interop_semaphore_handle semaphoreHandle,
640+
release_external_semaphore(interop_semaphore_handle semaphoreHandle,
641641
const sycl::queue &syclQueue) {
642-
destroy_external_semaphore(semaphoreHandle, syclQueue.get_device(),
642+
release_external_semaphore(semaphoreHandle, syclQueue.get_device(),
643643
syclQueue.get_context());
644644
}
645645

‎sycl/test-e2e/bindless_images/vulkan_interop/unsampled_images.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -134,9 +134,9 @@ create_test_handles(sycl::context &ctxt, sycl::device &dev,
134134
}
135135

136136
void cleanup_test(sycl::context &ctxt, sycl::device &dev, handles_t handles) {
137-
syclexp::destroy_external_semaphore(
137+
syclexp::release_external_semaphore(
138138
handles.sycl_wait_interop_semaphore_handle, dev, ctxt);
139-
syclexp::destroy_external_semaphore(
139+
syclexp::release_external_semaphore(
140140
handles.sycl_done_interop_semaphore_handle, dev, ctxt);
141141
syclexp::destroy_image_handle(handles.input_1, dev, ctxt);
142142
syclexp::destroy_image_handle(handles.input_2, dev, ctxt);

‎sycl/test/abi/pi_cuda_symbol_check.dump

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -106,14 +106,14 @@ piextCommandBufferUpdateKernelLaunch
106106
piextContextCreateWithNativeHandle
107107
piextContextGetNativeHandle
108108
piextContextSetExtendedDeleter
109-
piextDestroyExternalSemaphore
110109
piextDeviceCreateWithNativeHandle
111110
piextDeviceGetNativeHandle
112111
piextDeviceSelectBinary
113112
piextDisablePeerAccess
114113
piextEnablePeerAccess
115114
piextEnqueueCommandBuffer
116115
piextEnqueueCooperativeKernelLaunch
116+
piextEnqueueKernelLaunchCustom
117117
piextEnqueueNativeCommand
118118
piextEnqueueReadHostPipe
119119
piextEnqueueWriteHostPipe
@@ -157,6 +157,7 @@ piextProgramSetSpecializationConstant
157157
piextQueueCreate
158158
piextQueueCreateWithNativeHandle
159159
piextQueueGetNativeHandle
160+
piextReleaseExternalSemaphore
160161
piextSignalExternalSemaphore
161162
piextUSMDeviceAlloc
162163
piextUSMEnqueueFill
@@ -181,4 +182,3 @@ piextVirtualMemReserve
181182
piextVirtualMemSetAccess
182183
piextVirtualMemUnmap
183184
piextWaitExternalSemaphore
184-
piextEnqueueKernelLaunchCustom

‎sycl/test/abi/pi_hip_symbol_check.dump

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -106,7 +106,7 @@ piextCommandBufferUpdateKernelLaunch
106106
piextContextCreateWithNativeHandle
107107
piextContextGetNativeHandle
108108
piextContextSetExtendedDeleter
109-
piextDestroyExternalSemaphore
109+
piextReleaseExternalSemaphore
110110
piextDeviceCreateWithNativeHandle
111111
piextDeviceGetNativeHandle
112112
piextDeviceSelectBinary

‎sycl/test/abi/pi_level_zero_symbol_check.dump

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -105,14 +105,14 @@ piextCommandBufferUpdateKernelLaunch
105105
piextContextCreateWithNativeHandle
106106
piextContextGetNativeHandle
107107
piextContextSetExtendedDeleter
108-
piextDestroyExternalSemaphore
109108
piextDeviceCreateWithNativeHandle
110109
piextDeviceGetNativeHandle
111110
piextDeviceSelectBinary
112111
piextDisablePeerAccess
113112
piextEnablePeerAccess
114113
piextEnqueueCommandBuffer
115114
piextEnqueueCooperativeKernelLaunch
115+
piextEnqueueKernelLaunchCustom
116116
piextEnqueueNativeCommand
117117
piextEnqueueReadHostPipe
118118
piextEnqueueWriteHostPipe
@@ -156,6 +156,7 @@ piextProgramSetSpecializationConstant
156156
piextQueueCreate
157157
piextQueueCreateWithNativeHandle
158158
piextQueueGetNativeHandle
159+
piextReleaseExternalSemaphore
159160
piextSignalExternalSemaphore
160161
piextUSMDeviceAlloc
161162
piextUSMEnqueueFill
@@ -180,4 +181,3 @@ piextVirtualMemReserve
180181
piextVirtualMemSetAccess
181182
piextVirtualMemUnmap
182183
piextWaitExternalSemaphore
183-
piextEnqueueKernelLaunchCustom

‎sycl/test/abi/pi_nativecpu_symbol_check.dump

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -106,7 +106,7 @@ piextCommandBufferUpdateKernelLaunch
106106
piextContextCreateWithNativeHandle
107107
piextContextGetNativeHandle
108108
piextContextSetExtendedDeleter
109-
piextDestroyExternalSemaphore
109+
piextReleaseExternalSemaphore
110110
piextDeviceCreateWithNativeHandle
111111
piextDeviceGetNativeHandle
112112
piextDeviceSelectBinary

‎sycl/test/abi/pi_opencl_symbol_check.dump

Lines changed: 5 additions & 5 deletions
Original file line numberDiff line numberDiff line change
@@ -105,14 +105,14 @@ piextCommandBufferUpdateKernelLaunch
105105
piextContextCreateWithNativeHandle
106106
piextContextGetNativeHandle
107107
piextContextSetExtendedDeleter
108-
piextDestroyExternalSemaphore
109108
piextDeviceCreateWithNativeHandle
110109
piextDeviceGetNativeHandle
111110
piextDeviceSelectBinary
112111
piextDisablePeerAccess
113112
piextEnablePeerAccess
114113
piextEnqueueCommandBuffer
115114
piextEnqueueCooperativeKernelLaunch
115+
piextEnqueueKernelLaunchCustom
116116
piextEnqueueNativeCommand
117117
piextEnqueueReadHostPipe
118118
piextEnqueueWriteHostPipe
@@ -133,9 +133,6 @@ piextMemGetNativeHandle
133133
piextMemImageAllocate
134134
piextMemImageCopy
135135
piextMemImageCreateWithNativeHandle
136-
piextPhysicalMemCreate
137-
piextPhysicalMemRelease
138-
piextPhysicalMemRetain
139136
piextMemImageFree
140137
piextMemImageGetInfo
141138
piextMemMapExternalArray
@@ -147,6 +144,9 @@ piextMemSampledImageHandleDestroy
147144
piextMemUnsampledImageCreate
148145
piextMemUnsampledImageHandleDestroy
149146
piextPeerAccessGetInfo
147+
piextPhysicalMemCreate
148+
piextPhysicalMemRelease
149+
piextPhysicalMemRetain
150150
piextPlatformCreateWithNativeHandle
151151
piextPlatformGetNativeHandle
152152
piextPluginGetOpaqueData
@@ -156,6 +156,7 @@ piextProgramSetSpecializationConstant
156156
piextQueueCreate
157157
piextQueueCreateWithNativeHandle
158158
piextQueueGetNativeHandle
159+
piextReleaseExternalSemaphore
159160
piextSignalExternalSemaphore
160161
piextUSMDeviceAlloc
161162
piextUSMEnqueueFill
@@ -180,4 +181,3 @@ piextVirtualMemReserve
180181
piextVirtualMemSetAccess
181182
piextVirtualMemUnmap
182183
piextWaitExternalSemaphore
183-
piextEnqueueKernelLaunchCustom

‎sycl/test/abi/sycl_symbols_linux.dump

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -3045,8 +3045,8 @@ _ZN4sycl3_V13ext6oneapi12experimental25import_external_semaphoreINS3_21resource_
30453045
_ZN4sycl3_V13ext6oneapi12experimental25import_external_semaphoreINS3_21resource_win32_handleEEENS3_24interop_semaphore_handleENS3_29external_semaphore_descriptorIT_EERKNS0_6deviceERKNS0_7contextE
30463046
_ZN4sycl3_V13ext6oneapi12experimental25map_external_image_memoryENS3_18interop_mem_handleERKNS3_16image_descriptorERKNS0_5queueE
30473047
_ZN4sycl3_V13ext6oneapi12experimental25map_external_image_memoryENS3_18interop_mem_handleERKNS3_16image_descriptorERKNS0_6deviceERKNS0_7contextE
3048-
_ZN4sycl3_V13ext6oneapi12experimental26destroy_external_semaphoreENS3_24interop_semaphore_handleERKNS0_5queueE
3049-
_ZN4sycl3_V13ext6oneapi12experimental26destroy_external_semaphoreENS3_24interop_semaphore_handleERKNS0_6deviceERKNS0_7contextE
3048+
_ZN4sycl3_V13ext6oneapi12experimental26release_external_semaphoreENS3_24interop_semaphore_handleERKNS0_5queueE
3049+
_ZN4sycl3_V13ext6oneapi12experimental26release_external_semaphoreENS3_24interop_semaphore_handleERKNS0_6deviceERKNS0_7contextE
30503050
_ZN4sycl3_V13ext6oneapi12experimental4node12update_rangeILi1EEEvNS0_5rangeIXT_EEE
30513051
_ZN4sycl3_V13ext6oneapi12experimental4node12update_rangeILi2EEEvNS0_5rangeIXT_EEE
30523052
_ZN4sycl3_V13ext6oneapi12experimental4node12update_rangeILi3EEEvNS0_5rangeIXT_EEE

0 commit comments

Comments
 (0)