Skip to content

[SYCL][CUDA] Reduction ext unsupported - #1641

Merged
bader merged 1 commit into
intel:syclfrom
codeplaysoftware:bjoern/mark-reduction-extension-lit-tests-as-unsupported-by-cuda
May 6, 2020
Merged

[SYCL][CUDA] Reduction ext unsupported#1641
bader merged 1 commit into
intel:syclfrom
codeplaysoftware:bjoern/mark-reduction-extension-lit-tests-as-unsupported-by-cuda

Conversation

@bjoernknafla

Copy link
Copy Markdown

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
Copy Markdown
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

bader commented May 5, 2020

Copy link
Copy Markdown
Contributor

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
Copy Markdown
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

Ruyk commented May 6, 2020

Copy link
Copy Markdown
  • 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
Copy Markdown
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