Skip to content

Commit f157c1b

Browse files
authored
[SYCL][Bindless] Extend image copies (intel#16661)
Cleanup and extend image copies. * Cleanup and fix copy function comments * Update 'image_mem_handle' to 'image_mem_handle' to accept two image descriptors * Add support for USM to 'image_mem_handle' copies and sub-copies * Add support for 'image_mem_handle' to USM copies and sub-copies * Add support for USM to USM copies and sub-copies * Add support for host to host copies and sub-copies
1 parent cda8572 commit f157c1b

18 files changed

+3436
-1250
lines changed
Lines changed: 6 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -1,7 +1,7 @@
1-
# commit 8e6ea72e44dab71e976b3daf439073c4ef9a847b
2-
# Merge: 1f6945ce c57c181d
1+
# commit e2df8acd37c3c159364cfdf9dfdc1be35b71779e
2+
# Merge: 992ff37f 3a31ffee
33
# Author: Kenneth Benzie (Benie) <[email protected]>
4-
# Date: Wed Jan 29 15:54:56 2025 +0000
5-
# Merge pull request #2619 from martygrant/martin/memimage-info-unswitch-redo
6-
# Move urMemImageGetInfo success test from a switch to individual test
7-
set(UNIFIED_RUNTIME_TAG 8e6ea72e44dab71e976b3daf439073c4ef9a847b)
4+
# Date: Fri Jan 31 10:15:03 2025 +0000
5+
# Merge pull request #2575 from DBDuncan/duncan/extend-copies
6+
# [CUDA][Bindless] Add support for device to device pitched copies and host to host copies
7+
set(UNIFIED_RUNTIME_TAG e2df8acd37c3c159364cfdf9dfdc1be35b71779e)

sycl/doc/extensions/experimental/sycl_ext_oneapi_bindless_images.asciidoc

Lines changed: 275 additions & 43 deletions
Large diffs are not rendered by default.

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

Lines changed: 322 additions & 28 deletions
Large diffs are not rendered by default.

sycl/include/sycl/handler.hpp

Lines changed: 227 additions & 85 deletions
Large diffs are not rendered by default.

sycl/include/sycl/queue.hpp

Lines changed: 740 additions & 250 deletions
Large diffs are not rendered by default.

sycl/source/detail/memory_manager.cpp

Lines changed: 2 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -1644,7 +1644,8 @@ void MemoryManager::copy_image_bindless(
16441644
"Copy image bindless must be called with a valid device queue");
16451645
assert((Flags == UR_EXP_IMAGE_COPY_FLAG_HOST_TO_DEVICE ||
16461646
Flags == UR_EXP_IMAGE_COPY_FLAG_DEVICE_TO_HOST ||
1647-
Flags == UR_EXP_IMAGE_COPY_FLAG_DEVICE_TO_DEVICE) &&
1647+
Flags == UR_EXP_IMAGE_COPY_FLAG_DEVICE_TO_DEVICE ||
1648+
Flags == UR_EXP_IMAGE_COPY_FLAG_HOST_TO_HOST) &&
16481649
"Invalid flags passed to copy_image_bindless.");
16491650
if (!Dst || !Src)
16501651
throw sycl::exception(

0 commit comments

Comments
 (0)