Skip to content

[SYCL][Doc] Bindless Images proposal revision 4 #9842

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.

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

Merged
merged 6 commits into from
Jul 6, 2023

Conversation

ProGTX
Copy link
Contributor

@ProGTX ProGTX commented Jun 13, 2023

Replaces #8307

Required for #9808 and #10112 .

Addressed some of the feedback on revision 3 as revision 4. Any larger changes will need to move to subsequent revisions.

ProGTX and others added 3 commits June 13, 2023 13:23
Initial proposal for adding support for Bindless Images in SYCL.

Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
* Converted to ASCIIDOC
* Added `image_mem_handle` for image memory allocated with `allocate_image`
* Added ability to create images from USM
* Added new way to copy images, removed requirement for copy  direction
* Added image memory information getters to reflect `cuArray3DGetDescriptor` functionality
Co-authored-by: Przemyslaw Malon <przemek.malon@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>

- Some text clarifications.

- Unsampled images can no longer be created from USM.

- Added SYCL 1.2.1 `image_channel_order` and
  `image_channel_type` structs.

- Added `image_type` to enable construction of layered,
  mipmap, and cubemap images in the future.

- Added device information descriptors for querying pitched
  allocation size and alignment requirement.

- Added `ext_oneapi_copy` methods for the `sycl::handler`.

- `ext_oneapi_copy` functions now take the `Src` as the first
  parameter.

- Created `image_mem` as a RAII style class.

- Renamed `allocate_image` to `alloc_image_mem`

- `pitched_alloc_device` can now take an `image_descriptor`.

- Added interoperability features

- Added support to query bindless image and interoperability
  capabilities

- Added mipmap support
```c++
// Nearest/linear filtering between mip levels
template <typename DataT, typename CoordT>
DataT read_image(const sample_image_handle &ImageHandle,
Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

typo: sample_image_handle -> sampled_image_handle

Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

Good catch! Fixed

of the type of memory to be freed.

The `image_mem` class is a RAII class wrapper that performs allocation and
deallocation of device memory.
Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

Other SYCL memory objects, like buffer, also manage their memory objects, but still allow copies. Why do we want to break the mold with this new class, instead of marking it as having the common reference semantics?

Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

Our implementation currently does not follow CRS, and to re-design image_mem to follow PIMPL for copy-construction, and meet all other requirements for CRS might take more time than we have before the feature freeze date.

We do plan on making image_mem follow CRS in the next revision.

Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

We've managed to change the implementation of image_mem to follow common reference semantics, and have updated the proposal accordingly. The implementation of image_mem following CRS will pushed in our third PR after PR 2/4 is merged.

Co-authored-by: Isaac Ault isaac.ault@codeplay.com
Co-authored-by: Przemek Malon przemek.malon@codeplay.com
Co-authored-by: Sean Stirling sean.stirling@codeplay.com
Co-authored-by: Peter Zuzek peter@codeplay.com

- Added `sycl::device` parameter to multiple functions to
  clarify that images must be created and used on the same
  device.

- Changed naming and order of some parameters to be consistent
  throughout the proposal and with core SYCL.

- Added variants of functions that take a `sycl::queue`
  instead of both `sycl::device` and `sycl::context`.

- Removed standalone wait and signal semaphore functions. These
  should always go through the queue or handler methods.

- Removed `get_image_handle` and `get_sampler_handle` functions
  from sampled and unsampled image handle structs. The structs
  have public handle members that can be retrieved without
  getters.

- Made all enum types and values unspecified

- Moved support queries to device aspects, improved naming of
  queries for better consistency, and moved device info queries
  to the experimental namespace.

- Added `get_mip_level_desc` member function to
  `image_descriptor`

- Fixed `get_mip_level_mem_handle` prototype in `image_mem`,
  and added a standalone function.

- Removed `ext_oneapi_copy` variants that take `image_mem`,
  the user should retrieve the raw handle and pass that
  themselves.

- Removed `ext_oneapi_copy` variants that take a mip level,
  the user should retrieve individual mip level image handles
  themselves and pass that.

- Added `ext_oneapi_copy` variants that take offsets and the
  extent, to enable sub-region copy.

- Created a list of failure scenarios for `ext_oneapi_copy`,
  changed the failure error code to `errc::invalid`, and
  specified that the implementation should relay the reason
  for the failure back to the user.

- Added notes on the exception of using the SYCL 1.2.1
  `sampler` class, and reason for not using the SYCL 2020
  `image_sampler` struct.

- Updated code samples

- Other general improvements
Copy link
Contributor

@przemektmalon przemektmalon left a comment

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

We've updated the proposal to Revision 4, all prior existing feedback should be addressed, and we welcome new feedback on the Revision 4 additions and updates. See the revision history at the bottom of the document for an overview of the changes.

of the type of memory to be freed.

The `image_mem` class is a RAII class wrapper that performs allocation and
deallocation of device memory.
Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

Our implementation currently does not follow CRS, and to re-design image_mem to follow PIMPL for copy-construction, and meet all other requirements for CRS might take more time than we have before the feature freeze date.

We do plan on making image_mem follow CRS in the next revision.

```c++
// Nearest/linear filtering between mip levels
template <typename DataT, typename CoordT>
DataT read_image(const sample_image_handle &ImageHandle,
Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

Good catch! Fixed

@ProGTX ProGTX changed the title [SYCL][Doc] Bindless Images proposal revision 3 [SYCL][Doc] Bindless Images proposal revision 4 Jun 23, 2023
isaacault pushed a commit to codeplaysoftware/intel-llvm-mirror that referenced this pull request Jun 28, 2023
…s images extension

This commit stands as the second commit of four to make code review easier,
covering the changes made to the PI.

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>

Implement revision 4 of the bindless images extension proposal: intel#9842
@przemektmalon
Copy link
Contributor

Tagging @gmlueck @jbrodman @bashbaug


To represent the different sampling capabilities that mipmaps provide as opposed
to standard sampled images, we propose to extend the core SYCL `sampler`
class.
Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

The sampler class was removed with SYCL 2020 so we cannot and should not extend it. We could extend image_sampler but I would prefer we instead define a new sampler class to avoid the need to add ext_ to all the new members.

Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

Noted, we're working on removing the sycl::sampler extension and creating our own sampler struct. This will involve changes to our PR 2/4, hopefully removing the need for ABI-Break completely. We should have an update for the implementation and proposal soon.

Added a bindless_image_sampler struct to the proposal. We no longer
extend any existing SYCL samplers but use our own instead to avoid ABI
breaks.
`image_mem` has been specified that it now must follow Common Reference
Semantics as outlined by the core SYCL 2020 specification.
Copy link
Contributor

@steffenlarsen steffenlarsen left a comment

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

LGTM!

@steffenlarsen steffenlarsen merged commit 74e83d5 into intel:sycl Jul 6, 2023
przemektmalon pushed a commit to codeplaysoftware/intel-llvm-mirror that referenced this pull request Jul 18, 2023
…s images extension

This commit stands as the third commit of four to make code review easier,
mostly covering the changes made to the user-facing SYCL API for the
bindless images extension.

The bindless images extension provides a new interface for allocating,
creating, and accessing images in SYCL. Image memory allocation is
seperated from image handle creation, and image handles can be passed
to kernels without requesting access through accessors. This approach
provides much more flexibility to the user, as well as enabling programs
to implement features that were impossible to implement using standard
SYCL images, such as a texture atlas. In addition to providing a new
interface for images, this extension also provides initial experimental
support for importing external memory into SYCL.

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>

Implement revision 4 of the bindless images extension proposal: intel#9842
steffenlarsen pushed a commit that referenced this pull request Jul 18, 2023
…s images extension (#10112)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the second commit of four to make code review
easier, implementing revision 4 of the [bindless images extension
proposal](#9842).

## Scope

This PR covers changes made to the PI and the UR. This includes

- Extending PI with extension functions
- Updating UR FetchContent commit and implementing [UR bindless images
experimental
features](https://oneapi-src.github.io/unified-runtime/core/EXP-BINDLESS-IMAGES.html)
on the CUDA adaptor

## Following Split PRs

- [3/4] Implement the user-facing SYCL extension
- [4/4] Add tests

## Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
Seanst98 pushed a commit to codeplaysoftware/intel-llvm-mirror that referenced this pull request Jul 21, 2023
…s images extension

This commit stands as the fourth, and final, commit of four to make code
review easier, mostly covering the changes made to the e2e tests with the
additional tests for bindless images.

The bindless images extension provides a new interface for allocating,
creating, and accessing images in SYCL. Image memory allocation is
seperated from image handle creation, and image handles can be passed
to kernels without requesting access through accessors. This approach
provides much more flexibility to the user, as well as enabling programs
to implement features that were impossible to implement using standard
SYCL images, such as a texture atlas. In addition to providing a new
interface for images, this extension also provides initial experimental
support for importing external memory into SYCL.

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>

Implement revision 4 of the bindless images extension proposal:
intel#9842
steffenlarsen pushed a commit that referenced this pull request Jul 25, 2023
…s images extension (#10454)

This commit stands as the third commit of four to make code review
easier, mostly covering the changes made to the user-facing SYCL API for
the [bindless images extension
proposal](#9842).

### Overview

The bindless images extension provides a new interface for allocating,
creating, and accessing images in SYCL. Image memory allocation is
seperated from image handle creation, and image handles can be passed to
kernels without requesting access through accessors. This approach
provides much more flexibility to the user, as well as enabling programs
to implement features that were impossible to implement using standard
SYCL images, such as a texture atlas. In addition to providing a new
interface for images, this extension also provides initial experimental
support for importing external memory into SYCL.

### Following Split PRs

- [4/4] Add tests

### Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
steffenlarsen pushed a commit that referenced this pull request Aug 2, 2023
…CL bindless images extension (#10500)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the fourth, and final, commit of four to make code
review easier, covering the additional tests for bindless images to the
e2e test suite. Implementing [revision 4 of the bindless images
extension proposal](#9842).

This will not compile or run until
[PR3](#10454) has been merged.
However, it can be reviewed simultaneously with PR3.

## Overview

The bindless images extension provides a new interface for allocating,
creating, and accessing images in SYCL. Image memory allocation is
seperated from image handle creation, and image handles can be passed to
kernels without requesting access through accessors. This approach
provides much more flexibility to the user, as well as enabling programs
to implement features that were impossible to implement using standard
SYCL images, such as a texture atlas. In addition to providing a new
interface for images, this extension also provides initial experimental
support for importing external memory into SYCL.

## Previous PRs
* [1/4] [libclc](#9808)
* [2/4] [PI/UR](#10112)
* [3/4] [SYCL API](#10454)
* [4/4] Tests <--- This one

## Authors
Co-authored-by: Isaac Ault isaac.ault@codeplay.com
Co-authored-by: Hugh Bird hugh.bird@codeplay.com
Co-authored-by: Duncan Brawley duncan.brawley@codeplay.com
Co-authored-by: Przemek Malon przemek.malon@codeplay.com
Co-authored-by: Chedy Najjar chedy.najjar@codeplay.com
Co-authored-by: Sean Stirling sean.stirling@codeplay.com
Co-authored-by: Peter Zuzek peter@codeplay.com
Co-authored-by: SYCL Unbound Team <sycl.unbound@codeplay.com>
veselypeta pushed a commit to veselypeta/llvm that referenced this pull request Sep 21, 2023
…s images extension (intel#10112)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the second commit of four to make code review
easier, implementing revision 4 of the [bindless images extension
proposal](intel#9842).

## Scope

This PR covers changes made to the PI and the UR. This includes

- Extending PI with extension functions
- Updating UR FetchContent commit and implementing [UR bindless images
experimental
features](https://oneapi-src.github.io/unified-runtime/core/EXP-BINDLESS-IMAGES.html)
on the CUDA adaptor

## Following Split PRs

- [3/4] Implement the user-facing SYCL extension
- [4/4] Add tests

## Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
fabiomestre pushed a commit to fabiomestre/llvm that referenced this pull request Sep 26, 2023
…s images extension (intel#10112)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the second commit of four to make code review
easier, implementing revision 4 of the [bindless images extension
proposal](intel#9842).

## Scope

This PR covers changes made to the PI and the UR. This includes

- Extending PI with extension functions
- Updating UR FetchContent commit and implementing [UR bindless images
experimental
features](https://oneapi-src.github.io/unified-runtime/core/EXP-BINDLESS-IMAGES.html)
on the CUDA adaptor

## Following Split PRs

- [3/4] Implement the user-facing SYCL extension
- [4/4] Add tests

## Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
fabiomestre pushed a commit to fabiomestre/unified-runtime that referenced this pull request Sep 26, 2023
…s images extension (#10112)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the second commit of four to make code review
easier, implementing revision 4 of the [bindless images extension
proposal](intel/llvm#9842).

## Scope

This PR covers changes made to the PI and the UR. This includes

- Extending PI with extension functions
- Updating UR FetchContent commit and implementing [UR bindless images
experimental
features](https://oneapi-src.github.io/unified-runtime/core/EXP-BINDLESS-IMAGES.html)
on the CUDA adaptor

## Following Split PRs

- [3/4] Implement the user-facing SYCL extension
- [4/4] Add tests

## Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
fabiomestre pushed a commit to oneapi-src/unified-runtime that referenced this pull request Sep 27, 2023
…s images extension (#10112)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the second commit of four to make code review
easier, implementing revision 4 of the [bindless images extension
proposal](intel/llvm#9842).

## Scope

This PR covers changes made to the PI and the UR. This includes

- Extending PI with extension functions
- Updating UR FetchContent commit and implementing [UR bindless images
experimental
features](https://oneapi-src.github.io/unified-runtime/core/EXP-BINDLESS-IMAGES.html)
on the CUDA adaptor

## Following Split PRs

- [3/4] Implement the user-facing SYCL extension
- [4/4] Add tests

## Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
mdtoguchi pushed a commit to mdtoguchi/llvm that referenced this pull request Oct 18, 2023
…s images extension (intel#10454)

This commit stands as the third commit of four to make code review
easier, mostly covering the changes made to the user-facing SYCL API for
the [bindless images extension
proposal](intel#9842).

### Overview

The bindless images extension provides a new interface for allocating,
creating, and accessing images in SYCL. Image memory allocation is
seperated from image handle creation, and image handles can be passed to
kernels without requesting access through accessors. This approach
provides much more flexibility to the user, as well as enabling programs
to implement features that were impossible to implement using standard
SYCL images, such as a texture atlas. In addition to providing a new
interface for images, this extension also provides initial experimental
support for importing external memory into SYCL.

### Following Split PRs

- [4/4] Add tests

### Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
mdtoguchi pushed a commit to mdtoguchi/llvm that referenced this pull request Oct 18, 2023
…CL bindless images extension (intel#10500)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the fourth, and final, commit of four to make code
review easier, covering the additional tests for bindless images to the
e2e test suite. Implementing [revision 4 of the bindless images
extension proposal](intel#9842).

This will not compile or run until
[PR3](intel#10454) has been merged.
However, it can be reviewed simultaneously with PR3.

## Overview

The bindless images extension provides a new interface for allocating,
creating, and accessing images in SYCL. Image memory allocation is
seperated from image handle creation, and image handles can be passed to
kernels without requesting access through accessors. This approach
provides much more flexibility to the user, as well as enabling programs
to implement features that were impossible to implement using standard
SYCL images, such as a texture atlas. In addition to providing a new
interface for images, this extension also provides initial experimental
support for importing external memory into SYCL.

## Previous PRs
* [1/4] [libclc](intel#9808)
* [2/4] [PI/UR](intel#10112)
* [3/4] [SYCL API](intel#10454)
* [4/4] Tests <--- This one

## Authors
Co-authored-by: Isaac Ault isaac.ault@codeplay.com
Co-authored-by: Hugh Bird hugh.bird@codeplay.com
Co-authored-by: Duncan Brawley duncan.brawley@codeplay.com
Co-authored-by: Przemek Malon przemek.malon@codeplay.com
Co-authored-by: Chedy Najjar chedy.najjar@codeplay.com
Co-authored-by: Sean Stirling sean.stirling@codeplay.com
Co-authored-by: Peter Zuzek peter@codeplay.com
Co-authored-by: SYCL Unbound Team <sycl.unbound@codeplay.com>
omarahmed1111 pushed a commit to omarahmed1111/unified-runtime that referenced this pull request Oct 23, 2023
…s images extension (#10112)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the second commit of four to make code review
easier, implementing revision 4 of the [bindless images extension
proposal](intel/llvm#9842).

## Scope

This PR covers changes made to the PI and the UR. This includes

- Extending PI with extension functions
- Updating UR FetchContent commit and implementing [UR bindless images
experimental
features](https://oneapi-src.github.io/unified-runtime/core/EXP-BINDLESS-IMAGES.html)
on the CUDA adaptor

## Following Split PRs

- [3/4] Implement the user-facing SYCL extension
- [4/4] Add tests

## Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
omarahmed1111 pushed a commit to omarahmed1111/unified-runtime that referenced this pull request Oct 23, 2023
…s images extension (#10112)

# Experimental Implementation of SYCL Bindless Images Extension

This commit stands as the second commit of four to make code review
easier, implementing revision 4 of the [bindless images extension
proposal](intel/llvm#9842).

## Scope

This PR covers changes made to the PI and the UR. This includes

- Extending PI with extension functions
- Updating UR FetchContent commit and implementing [UR bindless images
experimental
features](https://oneapi-src.github.io/unified-runtime/core/EXP-BINDLESS-IMAGES.html)
on the CUDA adaptor

## Following Split PRs

- [3/4] Implement the user-facing SYCL extension
- [4/4] Add tests

## Authors

Co-authored-by: Isaac Ault <isaac.ault@codeplay.com>
Co-authored-by: Hugh Bird <hugh.bird@codeplay.com>
Co-authored-by: Duncan Brawley <duncan.brawley@codeplay.com>
Co-authored-by: Przemek Malon <przemek.malon@codeplay.com>
Co-authored-by: Chedy Najjar <chedy.najjar@codeplay.com>
Co-authored-by: Sean Stirling <sean.stirling@codeplay.com>
Co-authored-by: Peter Zuzek <peter@codeplay.com>
@ProGTX ProGTX deleted the bindless_rev3 branch August 9, 2024 09:24
Sign up for free to join this conversation on GitHub. Already have an account? Sign in to comment
Labels
None yet
Projects
None yet
Development

Successfully merging this pull request may close these issues.

4 participants