Add Frontend test

Author: AlexeySachkov

clang/test/Frontend/Inputs/sycl.hpp

@@ -0,0 +1,68 @@
+#pragma once
+
+#define ATTR_SYCL_KERNEL __attribute__((sycl_kernel))
+
+inline namespace cl {
+namespace sycl {
+
+// Dummy aspect enum with limited enumerators
+enum class aspect {
+  host = 0,
+  cpu = 1,
+  gpu = 2,
+  accelerator = 3,
+  custom = 4,
+  fp16 = 5,
+  fp64 = 6,
+};
+
+class kernel {};
+class context {};
+class device {};
+class event {};
+
+class queue {
+public:
+  template <typename T>
+  event submit(T cgf) { return event{}; }
+
+  void wait() {}
+  void wait_and_throw() {}
+  void throw_asynchronous() {}
+};
+
+class auto_name {};
+template <typename Name, typename Type>
+struct get_kernel_name_t {
+  using name = Name;
+};
+template <typename Type>
+struct get_kernel_name_t<auto_name, Type> {
+  using name = Type;
+};
+
+class kernel_handler {
+  void __init_specialization_constants_buffer(char *specialization_constants_buffer) {}
+};
+
+#define ATTR_SYCL_KERNEL __attribute__((sycl_kernel))
+template <typename KernelName, typename KernelType>
+ATTR_SYCL_KERNEL void kernel_single_task(const KernelType &kernelFunc) { // #KernelSingleTask
+  kernelFunc();
+}
+
+class handler {
+public:
+  template <typename KernelName = auto_name, typename KernelType>
+  void single_task(const KernelType &kernelFunc) {
+    using NameT = typename get_kernel_name_t<KernelName, KernelType>::name;
+#ifdef __SYCL_DEVICE_ONLY__
+    kernel_single_task<NameT>(kernelFunc);
+#else
+    kernelFunc();
+#endif
+  }
+};
+
+} // namespace sycl
+} // namespace cl

clang/test/Frontend/sycl-aspects-usage.cpp

@@ -0,0 +1,42 @@
+// Test checks Propagate Aspect Usage pass.
+
+// RUN: %clang_cc1 -fsycl-is-device -triple spir64-unknown-unknown -emit-llvm %s -o /dev/null 2>&1 | FileCheck %s --check-prefix CHECK-WARNINGS
+
+// RUNx: %clang_cc1 -fsycl-is-device -triple spir64-unknown-unknown %s -debug-info-kind=constructor -dwarf-version=5 -emit-llvm -o /dev/null 2>&1 | FileCheck %s --check-prefix CHECK-WARNINGS-DBG -DPATH=%s
+
+// CHECK-WARNINGS: warning: function 'func1(int)' uses aspect 'fp16' not listed in 'sycl::device_has()'
+// CHECK-WARNINGS-NEXT: note: the actual use is in func3(int, int, int), compile with '-g' to get source location
+// CHECK-WARNINGS-NEXT: note: which is called by func2(int, int), compile with '-g' to get source location
+// CHECK-WARNINGS-NEXT: note: which is called by func1(int), compile with '-g' to get source location
+//
+// CHECK-WARNINGS-DBG: warning: function 'func1(int)' uses aspect 'fp16' not listed in 'sycl::device_has()'
+// CHECK-WARNINGS-DBG-NEXT: note: the actual use is in func3(int, int, int) at [[PATH]]:36:5
+// CHECK-WARNINGS-DBG-NEXT: note: which is called by func2(int, int) at [[PATH]]:40:34
+// CHECK-WARNINGS-DBG-NEXT: note: which is called by func1(int) at [[PATH]]:42:62
+
+#include "Inputs/sycl.hpp"
+
+using namespace cl::sycl;
+
+class KernelName;
+
+struct [[__sycl_detail__::__uses_aspects__(aspect::fp16)]] Struct {
+  int a = 0;
+};
+
+int func3(int a, int b, int c) {
+  Struct s;
+  s.a = 1;
+  return s.a;
+}
+
+int func2(int a, int b) { return func3(a, b, 1); }
+
+[[sycl::device_has(aspect::fp64)]] int func1(int a) { return func2(a, 1); }
+
+int main() {
+  queue Q;
+  Q.submit([&](handler &h) {
+    h.single_task<KernelName>([=]() { int a = func1(1); });
+  });
+}