Skip to content

[SYCL][ESIMD] Add support for local accessors to lsc API #10340

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 8 commits into from
Jul 28, 2023

Conversation

fineg74
Copy link
Contributor

@fineg74 fineg74 commented Jul 12, 2023

No description provided.

@fineg74 fineg74 requested a review from a team as a code owner July 12, 2023 23:33
@fineg74 fineg74 temporarily deployed to aws July 12, 2023 23:46 — with GitHub Actions Inactive
@fineg74 fineg74 temporarily deployed to aws July 13, 2023 00:30 — with GitHub Actions Inactive
@fineg74 fineg74 temporarily deployed to aws July 13, 2023 02:32 — with GitHub Actions Inactive
@fineg74 fineg74 temporarily deployed to aws July 13, 2023 03:09 — with GitHub Actions Inactive
Copy link
Contributor

@turinevgeny turinevgeny left a comment

Choose a reason for hiding this comment

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

Mostly LGTM, just a couple of questions.

@fineg74 fineg74 temporarily deployed to aws July 25, 2023 01:09 — with GitHub Actions Inactive
@fineg74 fineg74 temporarily deployed to aws July 25, 2023 01:48 — with GitHub Actions Inactive
@fineg74 fineg74 temporarily deployed to aws July 27, 2023 00:54 — with GitHub Actions Inactive
@fineg74 fineg74 temporarily deployed to aws July 27, 2023 01:54 — with GitHub Actions Inactive
!std::is_same_v<Toffset, uint64_t>,
__ESIMD_NS::simd<T, N * NElts>>
__ESIMD_API std::enable_if_t<
!std::is_pointer_v<AccessorTy> &&
Copy link
Contributor

Choose a reason for hiding this comment

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

Just a note here:
!std::is_pointer_v is a bad check (not because of your PR). It allows using write-only accessors lsc_gather() operations. Same/vice-versa is for read-only accessors usable in write operations in other places in memory.hpp here.

I created internal tracker for this issue.

Copy link
Contributor

Choose a reason for hiding this comment

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

The much better check is used for copy_to() and copy_from(), e.g. copy_from():

detail::is_sycl_accessor_with<
                     AccessorT, accessor_mode_cap::can_read,
                     sycl::access::target::device>::value)

@v-klochkov v-klochkov merged commit 9dce2d2 into intel:sycl Jul 28, 2023
@fineg74 fineg74 deleted the localAccessorLSC branch July 28, 2023 02:42
mdtoguchi pushed a commit to mdtoguchi/llvm that referenced this pull request Oct 18, 2023
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.

3 participants