From e9f1c5c16afd5eff96c7f9f26972b55b9fa14915 Mon Sep 17 00:00:00 2001 From: Sergey V Maslov Date: Fri, 15 Jan 2021 21:34:38 -0800 Subject: [PATCH 1/4] [SYCL] test for barrier submission: https://github.com/intel/llvm/pull/3045 Signed-off-by: Sergey V Maslov --- SYCL/Basic/submit_barrier.cpp | 17 +++++++++++++++++ 1 file changed, 17 insertions(+) create mode 100755 SYCL/Basic/submit_barrier.cpp diff --git a/SYCL/Basic/submit_barrier.cpp b/SYCL/Basic/submit_barrier.cpp new file mode 100755 index 0000000000..368449358b --- /dev/null +++ b/SYCL/Basic/submit_barrier.cpp @@ -0,0 +1,17 @@ +// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple %s -o %t.out +// RUN: %HOST_RUN_PLACEHOLDER %t.out +// RUN: %CPU_RUN_PLACEHOLDER %t.out +// RUN: %GPU_RUN_PLACEHOLDER %t.out + +#include +#include + +int main() { + cl::sycl::device dev; + cl::sycl::queue q{dev}; + + cl::sycl::event e = q.submit_barrier(); + e.wait_and_throw(); + + return 0; +} From f128bec4904bae4e104928cb9e7dd48059f6c926 Mon Sep 17 00:00:00 2001 From: Sergey V Maslov Date: Thu, 21 Jan 2021 14:55:12 -0800 Subject: [PATCH 2/4] use default device selector Signed-off-by: Sergey V Maslov --- SYCL/Basic/submit_barrier.cpp | 8 ++++++-- 1 file changed, 6 insertions(+), 2 deletions(-) diff --git a/SYCL/Basic/submit_barrier.cpp b/SYCL/Basic/submit_barrier.cpp index 368449358b..fc827b4400 100755 --- a/SYCL/Basic/submit_barrier.cpp +++ b/SYCL/Basic/submit_barrier.cpp @@ -1,4 +1,4 @@ -// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple %s -o %t.out +// RUN: %clangxx -fsycl %s -o %t.out // RUN: %HOST_RUN_PLACEHOLDER %t.out // RUN: %CPU_RUN_PLACEHOLDER %t.out // RUN: %GPU_RUN_PLACEHOLDER %t.out @@ -7,9 +7,13 @@ #include int main() { - cl::sycl::device dev; + + cl::sycl::device dev{cl::sycl::default_selector{}}; cl::sycl::queue q{dev}; + q.submit( + [&](sycl::handler &cgh) { cgh.single_task([]() {}); }); + cl::sycl::event e = q.submit_barrier(); e.wait_and_throw(); From 5fd63038a7dd8e2aa252d02b7f06923b1779dce9 Mon Sep 17 00:00:00 2001 From: Sergey V Maslov Date: Sun, 14 Feb 2021 18:13:27 -0800 Subject: [PATCH 3/4] add -fsycl-targets Signed-off-by: Sergey V Maslov --- SYCL/Basic/submit_barrier.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/SYCL/Basic/submit_barrier.cpp b/SYCL/Basic/submit_barrier.cpp index fc827b4400..f7a64f93e9 100755 --- a/SYCL/Basic/submit_barrier.cpp +++ b/SYCL/Basic/submit_barrier.cpp @@ -1,4 +1,4 @@ -// RUN: %clangxx -fsycl %s -o %t.out +// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple %s -o %t.out // RUN: %HOST_RUN_PLACEHOLDER %t.out // RUN: %CPU_RUN_PLACEHOLDER %t.out // RUN: %GPU_RUN_PLACEHOLDER %t.out From 6c510c16568f09027c94bac356235a274842b799 Mon Sep 17 00:00:00 2001 From: Sergey V Maslov Date: Sun, 14 Feb 2021 18:52:31 -0800 Subject: [PATCH 4/4] disable for CUDA Signed-off-by: Sergey V Maslov --- SYCL/Basic/submit_barrier.cpp | 2 ++ 1 file changed, 2 insertions(+) diff --git a/SYCL/Basic/submit_barrier.cpp b/SYCL/Basic/submit_barrier.cpp index f7a64f93e9..eae0866976 100755 --- a/SYCL/Basic/submit_barrier.cpp +++ b/SYCL/Basic/submit_barrier.cpp @@ -3,6 +3,8 @@ // RUN: %CPU_RUN_PLACEHOLDER %t.out // RUN: %GPU_RUN_PLACEHOLDER %t.out +// UNSUPPORTED: cuda + #include #include