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] Reduction ext unsupported #1641

Conversation

bjoernknafla
Copy link
Contributor

The reduction extension is not yet supported by CUDA. Mark LIT tests as
unsupported.

Signed-off-by: Bjoern Knafla bjoern@codeplay.com

@bjoernknafla bjoernknafla requested a review from a team as a code owner May 5, 2020 11:22
@bjoernknafla bjoernknafla requested a review from vladimirlaz May 5, 2020 11:22
@v-klochkov
Copy link
Contributor

The reduction extension is not yet supported by CUDA. Mark LIT tests as
unsupported.

Signed-off-by: Bjoern Knafla bjoern@codeplay.com

I have one question and 1 comment:

  1. When these 2 big patches were merged all tests reported passes.
    [SYCL] Implement basic reduction for parallel_for() accepting nd_range #1585
    [SYCL] Add faster reduction implementations using atomic or/and intel… #1615
    Do you think CUDA testing was turned OFF in CI in those days, or something changed in CUDA testing settings?

  2. reduction feature only uses other existing sycl features. 3 basic features used by reduction:

  • parallel_for accepting nd_range. (Is that supported on CUDA?)
  • sycl::atomic class and operations like fetch_add(), fetch_min(), etc. (same question)
  • intel::reduce() algorithm

In the lines:
// UNSUPPORTED: cuda
would you please be more specific. For example:
// UNSUPPORTED: cuda
// cuda does not yet support sycl::atomic, intel::reduce() features used by reduction implementation

@bader
Copy link
Contributor

bader commented May 5, 2020

If these tests are not working due to the bugs rather than unsupported features than we should probably disable them using XFAIL instead of UNSUPPORTED.

@vladimirlaz
Copy link
Contributor

The reduction extension is not yet supported by CUDA. Mark LIT tests as
unsupported.
Signed-off-by: Bjoern Knafla bjoern@codeplay.com

I have one question and 1 comment:

  1. When these 2 big patches were merged all tests reported passes.
    [SYCL] Implement basic reduction for parallel_for() accepting nd_range #1585
    [SYCL] Add faster reduction implementations using atomic or/and intel… #1615
    Do you think CUDA testing was turned OFF in CI in those days, or something changed in CUDA testing settings?

@Ruyk
Copy link
Contributor

Ruyk commented May 6, 2020

  • intel::reduce() algorithm

Intel reduce algorithm is not a standard or "basic" SYCL feature. We are implementing SYCL 1.2.1 features first.

In the lines:
// UNSUPPORTED: cuda
would you please be more specific. For example:
// UNSUPPORTED: cuda
// cuda does not yet support sycl::atomic, intel::reduce() features used by reduction implementation

Atomic should be there once we finish the work on builtins.
Reduction is on the roadmap for later, but not implemented yet. Makes sense to clarify that on the comment.

The reduction extension is not yet supported by CUDA. Mark LIT tests as
unsupported.

Signed-off-by: Bjoern Knafla <bjoern@codeplay.com>
@bjoernknafla
Copy link
Contributor Author

Good call to document why the tests are unsupported. It is due to OpenCL 2.x alike work-group builtins which the CUDA implementation is not supporting yet. I will add the description to the tests.

@bjoernknafla bjoernknafla force-pushed the bjoern/mark-reduction-extension-lit-tests-as-unsupported-by-cuda branch from 1f53af0 to f1f3f6a Compare May 6, 2020 14:12
@bader bader added the cuda CUDA back-end label May 6, 2020
@bader bader merged commit 16d866b into intel:sycl May 6, 2020
alexbatashev pushed a commit to alexbatashev/llvm that referenced this pull request May 7, 2020
…xmethods

* origin/sycl:
  [SYCL][CUDA] Reduction ext unsupported (intel#1641)
  [SYCL][NFC] Simplifying contribution guidelines (intel#1644)
alexbatashev pushed a commit to alexbatashev/llvm that referenced this pull request May 7, 2020
…_docs

* origin/sycl:
  [SYCL] Fix xmethod script deployment (intel#1645)
  [SYCL] Support scalar accessor in handler::copy(acc,ptr) and copy(ptr,acc) (intel#1634)
  [SYCL][CUDA] Reduction ext unsupported (intel#1641)
  [SYCL][NFC] Simplifying contribution guidelines (intel#1644)
@bjoernknafla bjoernknafla deleted the bjoern/mark-reduction-extension-lit-tests-as-unsupported-by-cuda branch May 7, 2020 14:53
Sign up for free to join this conversation on GitHub. Already have an account? Sign in to comment
Labels
cuda CUDA back-end
Projects
None yet
Development

Successfully merging this pull request may close these issues.

5 participants