Merge branch 'intel' into private/MrSidims/UpdateCODEOWNERS

Author: bader

.github/CODEOWNERS

@@ -1,86 +1,35 @@
 * @vladimirlaz @romanovvlad @bader
 
-# AOT compilation
-SYCL/AOT @AGindinson @dm-vodopyanov @AlexeySachkov @romanovvlad
+# Use runtime team as the umbrella for most of the tests
+/SYCL/ @intel/llvm-reviewers-runtime
 
-# Atomics
-SYCL/AtomicRef @AGindinson 
 
-# SYCL RT specific tests
-SYCL/Assert @intel/llvm-reviewers-runtime
-SYCL/Basic @intel/llvm-reviewers-runtime
-SYCL/Config @intel/llvm-reviewers-runtime
-SYCL/DiscardEvents @intel/llvm-reviewers-runtime
-SYCL/FilterSelector @intel/llvm-reviewers-runtime
-SYCL/HostInteropTask @intel/llvm-reviewers-runtime
-SYCL/InorderQueue @intel/llvm-reviewers-runtime
-SYCL/KernelAndProgram @intel/llvm-reviewers-runtime
-SYCL/KernelParams @intel/llvm-reviewers-runtime
-SYCL/Scheduler @intel/llvm-reviewers-runtime
-SYCL/Tracing  @intel/llvm-reviewers-runtime
-
-# Device code split
-SYCL/DeviceCodeSplit @AlexeySachkov  @Fznamznon
-
-# Device library
-SYCL/DeviceLib @vzakhari
-SYCL/DeviceLib/ITTAnnotations @vzakhari @MrSidims @AGindinson
-
-# dot_product API
-SYCL/DotProduct @rdeodhar
-
-# Explicit SIMD
-SYCL/ESIMD @kbobrovs @v-klochkov @sndmitriev
-
-# Functor
-SYCL/Functor @AlexeySachkov
+# SYCL sub-directory matchers are grouped by code owner first, followed by
+# alphabetical order within the group. Please, keep this ordering.
 
 # Group algorithms
-SYCL/GroupAlgorithm @Pennycook @AlexeySachkov
-SYCL/SubGroup @Pennycook @AlexeySachkov
-SYCL/SubGroupMask @Pennycook @vladimirlaz
 
-# Group local memory
-SYCL/GroupLocalMemory @sergey-semenov @Pennycook
+/SYCL/GroupAlgorithm/ @Pennycook @intel/llvm-reviewers-runtime
+/SYCL/GroupLocalMemory/ @Pennycook @intel/llvm-reviewers-runtime
+/SYCL/SubGroup/ @Pennycook @intel/llvm-reviewers-runtime
+/SYCL/SubGroupMask/ @Pennycook @intel/llvm-reviewers-runtime
 
-# Hierarchical parallelism
-SYCL/HierPar @kbobrovs
+# Plugin interface for Level Zero
+/SYCL/Plugin/*level[-_]zero* @intel/dpcpp-l0-pi-reviewers
 
-# Inline assembler
-SYCL/InlineAsm @AlexeySachkov
+# Explicit SIMD
+/SYCL/ESIMD/ @intel/dpcpp-esimd-reviewers
 
-# Online compiler
-SYCL/OnlineCompiler @v-klochkov
+# BFloat16 conversion
+/SYCL/BFloat16/ @AlexeySotkin @intel/dpcpp-tools-reviewers
 
-# Plugin interface
-SYCL/Plugin @smaslov-intel
+# Compiler tests
+/SYCL/AOT/ @intel/dpcpp-tools-reviewers
+/SYCL/DeviceCodeSplit/ @intel/dpcpp-tools-reviewers
+/SYCL/SeparateCompile/ @intel/dpcpp-tools-reviewers
 
 # Printf
-SYCL/Printf @AlexeySachkov @AGindinson @mlychkov
-
-# Reduction algorithms
-SYCL/Reduction @v-klochkov
-
-# Image sampler
-SYCL/Sampler @cperkinsintel
-
-# Separate compilation
-SYCL/SeparateCompile @AlexeySachkov  @Fznamznon
+/SYCL/Printf/ @intel/dpcpp-tools-reviewers
 
 # Specialization constant
-SYCL/SpecConstants @kbobrovs
-
-# Unified Shared Memory (USM)
-SYCL/USM @jbrodman @sergey-semenov
-
-# Stream
-SYCL/Basic/stream @againull
-
-#BFloat16 conversion
-SYCL/BFloat16 @MrSidims
-
-# Deprecated features
-SYCL/DeprecatedFeatures @intel/llvm-reviewers-runtime
-
-# XPTI and XPTI Framework
-SYCL/XPTI @intel/llvm-reviewers-runtime
+/SYCL/SpecConstants/ @intel/dpcpp-tools-reviewers

.github/workflows/clang-format.yml

@@ -8,22 +8,21 @@ on:
 jobs:
   build:
     runs-on: ubuntu-latest
-    steps:
-    - name: Get clang-format first
-      run: sudo apt-get install -yqq clang-format-9
 
+    container:
+      image: ghcr.io/intel/llvm/sycl_ubuntu2004_nightly:no-drivers
+
+    steps:
     - uses: actions/checkout@v2
       with:
         fetch-depth: 2
-
-    - name: Get clang-format-diff.py tool
-      run: |
-        wget https://raw.githubusercontent.com/intel/llvm/sycl/clang/tools/clang-format/clang-format-diff.py
-        chmod u+x clang-format-diff.py
 
     - name: Run clang-format for the patch
+      shell: bash {0}
       run: |
-        git diff -U0 --no-color ${GITHUB_SHA}^1 ${GITHUB_SHA} -- | python clang-format-diff.py -p1 -binary clang-format-9 > ./clang-format.patch
+        git clang-format ${GITHUB_SHA}^1
+        git diff > ./clang-format.patch
+
     # Add patch with formatting fixes to CI job artifacts
     - uses: actions/upload-artifact@v1
       with:

.gitignore

@@ -2,3 +2,4 @@
 # External/*
 /test-suite-externals
 *.pyc
+/build*

SYCL/AOT/accelerator.cpp

@@ -1,12 +1,12 @@
-//==--- accelerator.cpp - AOT compilation for fpga devices using aoc ------==//
+//=-- accelerator.cpp - compilation for fpga emulator dev using opencl-aot --=//
 //
 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
 // See https://llvm.org/LICENSE.txt for license information.
 // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
 //
 //===---------------------------------------------------------------------===//
 
-// REQUIRES: aoc, accelerator
+// REQUIRES: opencl-aot, accelerator
 
 // RUN: %clangxx -fsycl -fsycl-targets=spir64_fpga %S/Inputs/aot.cpp -o %t.out
 // RUN: %ACC_RUN_PLACEHOLDER %t.out

SYCL/AOT/multiple-devices.cpp

@@ -6,7 +6,7 @@
 //
 //===----------------------------------------------------------------------===//
 
-// REQUIRES: opencl-aot, ocloc, aoc, cpu, gpu, accelerator
+// REQUIRES: opencl-aot, ocloc, cpu, gpu, accelerator
 // UNSUPPORTED: cuda
 // CUDA is not compatible with SPIR.
 

SYCL/Assert/assert_in_kernels.cpp

@@ -1,7 +1,7 @@
 // REQUIRES: linux
 // FIXME unsupported on CUDA and HIP until fallback libdevice becomes available
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 // RUN: %GPU_RUN_PLACEHOLDER %t.out &> %t.txt || true

SYCL/Assert/assert_in_kernels_win.cpp

@@ -1,6 +1,6 @@
 // REQUIRES: windows
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 // RUN: %GPU_RUN_PLACEHOLDER %t.out &> %t.txt || true

SYCL/Assert/assert_in_multiple_tus.cpp

@@ -1,7 +1,7 @@
 // REQUIRES: linux
 // FIXME unsupported on CUDA and HIP until fallback libdevice becomes available
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple -I %S/Inputs %s %S/Inputs/kernels_in_file2.cpp -o %t.out
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple -I %S/Inputs %s %S/Inputs/kernels_in_file2.cpp -o %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 // RUN: %GPU_RUN_PLACEHOLDER %t.out &> %t.txt || true

SYCL/Assert/assert_in_multiple_tus_one_ndebug.cpp

@@ -1,7 +1,7 @@
 // REQUIRES: linux
 // FIXME unsupported on CUDA and HIP until fallback libdevice becomes available
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple -DDEFINE_NDEBUG_INFILE2 -I %S/Inputs %S/assert_in_multiple_tus.cpp %S/Inputs/kernels_in_file2.cpp -o %t.out
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple -DDEFINE_NDEBUG_INFILE2 -I %S/Inputs %S/assert_in_multiple_tus.cpp %S/Inputs/kernels_in_file2.cpp -o %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 // RUN: %GPU_RUN_PLACEHOLDER %t.out &> %t.txt || true

SYCL/Assert/assert_in_multiple_tus_one_ndebug_win.cpp

@@ -1,6 +1,6 @@
 // REQUIRES: windows
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple -DDEFINE_NDEBUG_INFILE2 -I %S/Inputs %S/assert_in_multiple_tus.cpp %S/Inputs/kernels_in_file2.cpp -o %t.out
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple -DDEFINE_NDEBUG_INFILE2 -I %S/Inputs %S/assert_in_multiple_tus.cpp %S/Inputs/kernels_in_file2.cpp -o %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 // RUN: %GPU_RUN_PLACEHOLDER %t.out &> %t.txt || true

SYCL/Assert/assert_in_multiple_tus_win.cpp

@@ -1,6 +1,6 @@
 // REQUIRES: windows
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple -I %S/Inputs %s %S/Inputs/kernels_in_file2.cpp -o %t.out
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple -I %S/Inputs %s %S/Inputs/kernels_in_file2.cpp -o %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 // RUN: %GPU_RUN_PLACEHOLDER %t.out &> %t.txt || true

SYCL/Assert/assert_in_one_kernel.cpp

@@ -1,7 +1,7 @@
 // REQUIRES: linux
 // FIXME unsupported on CUDA and HIP until fallback libdevice becomes available
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 // RUN: %GPU_RUN_PLACEHOLDER %t.out &> %t.txt || true

SYCL/Assert/assert_in_one_kernel_win.cpp

@@ -1,6 +1,6 @@
 // REQUIRES: windows
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 // RUN: %GPU_RUN_PLACEHOLDER %t.out &> %t.txt || true

SYCL/Assert/assert_in_simultaneous_kernels.cpp

@@ -1,7 +1,7 @@
 // REQUIRES: linux
 // FIXME unsupported on CUDA and HIP until fallback libdevice becomes available
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple %s -o %t.out %threads_lib
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple %s -o %t.out %threads_lib
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 //

SYCL/Assert/assert_in_simultaneous_kernels_win.cpp

@@ -1,6 +1,6 @@
 // REQUIRES: windows
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple %s -o %t.out %threads_lib
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple %s -o %t.out %threads_lib
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 //

SYCL/Assert/assert_in_simultaneously_multiple_tus.cpp

@@ -1,6 +1,6 @@
 // FIXME unsupported on CUDA and HIP until fallback libdevice becomes available
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple -I %S/Inputs %s %S/Inputs/kernels_in_file2.cpp -o %t.out %threads_lib
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple -I %S/Inputs %s %S/Inputs/kernels_in_file2.cpp -o %t.out %threads_lib
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 //

SYCL/Assert/assert_in_simultaneously_multiple_tus_one_ndebug.cpp

@@ -1,6 +1,6 @@
 // FIXME unsupported on CUDA and HIP until fallback libdevice becomes available
 // UNSUPPORTED: cuda || hip
-// RUN: %clangxx -DSYCL_ENABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple -DDEFINE_NDEBUG_INFILE2 -I %S/Inputs %S/assert_in_simultaneously_multiple_tus.cpp %S/Inputs/kernels_in_file2.cpp -o %t.out %threads_lib
+// RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%sycl_triple -DDEFINE_NDEBUG_INFILE2 -I %S/Inputs %S/assert_in_simultaneously_multiple_tus.cpp %S/Inputs/kernels_in_file2.cpp -o %t.out %threads_lib
 // RUN: %CPU_RUN_PLACEHOLDER %t.out &> %t.txt || true
 // RUN: %CPU_RUN_PLACEHOLDER FileCheck %s --input-file %t.txt
 //

SYCL/AtomicRef/add.cpp

@@ -1,44 +1,12 @@
-// RUN: %clangxx -fsycl -fsycl-unnamed-lambda -fsycl-targets=%sycl_triple %s -o %t.out \
-// RUN: -Xsycl-target-backend=nvptx64-nvidia-cuda --cuda-gpu-arch=sm_60
+// See https://github.com/intel/llvm-test-suite/issues/867 for detailed status
+// UNSUPPORTED: hip
+
+// RUN: %clangxx -fsycl -fsycl-unnamed-lambda -fsycl-device-code-split=per_kernel -fsycl-targets=%sycl_triple %s -o %t.out -Xsycl-target-backend=nvptx64-nvidia-cuda --cuda-gpu-arch=sm_70
 // RUN: %HOST_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %ACC_RUN_PLACEHOLDER %t.out
 
 #include "add.h"
-#include <iostream>
-using namespace sycl;
-
-// Floating-point types do not support pre- or post-increment
-template <> void add_test<float>(queue q, size_t N) {
-  add_fetch_test<::sycl::ext::oneapi::atomic_ref,
-                 access::address_space::global_space, float>(q, N);
-  add_fetch_test<::sycl::atomic_ref, access::address_space::global_space,
-                 float>(q, N);
-  add_plus_equal_test<::sycl::ext::oneapi::atomic_ref,
-                      access::address_space::global_space, float>(q, N);
-  add_plus_equal_test<::sycl::atomic_ref, access::address_space::global_space,
-                      float>(q, N);
-}
-
-int main() {
-  queue q;
-
-  constexpr int N = 32;
-  add_test<int>(q, N);
-  add_test<unsigned int>(q, N);
-  add_test<float>(q, N);
-
-  // Include long tests if they are 32 bits wide
-  if constexpr (sizeof(long) == 4) {
-    add_test<long>(q, N);
-    add_test<unsigned long>(q, N);
-  }
-
-  // Include pointer tests if they are 32 bits wide
-  if constexpr (sizeof(char *) == 4) {
-    add_test<char *, ptrdiff_t>(q, N);
-  }
 
-  std::cout << "Test passed." << std::endl;
-}
+int main() { add_test_all<access::address_space::global_space>(); }