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.

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

[SYCL][CUDA][LIT] Fix base address get and subbuffer LIT test #1913

Conversation

przemektmalon
Copy link
Contributor

This commit fixes a hardcoded value for base address alignment
in the CUDA backend. Also a hardcoded value that should be
dependant on the base address alignment is fixed in the subbuffer
LIT test, which now passes on CUDA.

Signed-off-by: Przemek Malon [email protected]

@przemektmalon przemektmalon requested review from a team as code owners June 17, 2020 06:18
@przemektmalon przemektmalon force-pushed the przemek/cuda-fix-base-addr-info-and-subbuffer-lit branch from 446ede1 to 1747afe Compare June 17, 2020 06:25
This commit fixes a hardcoded value for base address alignment
in the cuda backend. Also a hardcoded value that should be
dependant on the base address alignment is fixed in the subbuffer
LIT test, which now passes on CUDA.

Signed-off-by: Przemek Malon <[email protected]>
@przemektmalon przemektmalon force-pushed the przemek/cuda-fix-base-addr-info-and-subbuffer-lit branch from 1747afe to 788ac4e Compare June 17, 2020 14:37
@romanovvlad
Copy link
Contributor

@fwyzard FYI

@romanovvlad
Copy link
Contributor

@Ruyk Could you please take a look?

@@ -1,6 +1,3 @@
// XFAIL: cuda
Copy link
Contributor

Choose a reason for hiding this comment

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

This makes me happy!

cl::sycl::detail::pi::assertion(
cuDeviceGetAttribute(&mem_base_addr_align,
CU_DEVICE_ATTRIBUTE_TEXTURE_ALIGNMENT,
device->get()) == CUDA_SUCCESS);
Copy link
Contributor

Choose a reason for hiding this comment

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

Przemek and I discussed offline - the reported value aligns with the hard-coded value before. This alignment is probably required to enable creation of images, e.g., CL_MEM_OBJECT_IMAGE1D_BUFFER, from sub-buffers.

@bjoernknafla
Copy link
Contributor

+1

@bader bader merged commit a6d03f3 into intel:sycl Jun 19, 2020
@przemektmalon przemektmalon deleted the przemek/cuda-fix-base-addr-info-and-subbuffer-lit branch June 22, 2020 16:08
bb-sycl pushed a commit that referenced this pull request Apr 4, 2023
Extension name will be preserved for a while for binary compatibility.

Signed-off-by: Sidorov, Dmitry <[email protected]>

Original commit:
KhronosGroup/SPIRV-LLVM-Translator@68855f6
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.

5 participants