[SYCL] Add check for generated PDBs (intel#554)

Author: vladimirlaz

SYCL/PDB/sycl.cpp

@@ -0,0 +1,22 @@
+// REQUIRES: windows,timelimit,(opencl||level_zero)
+// RUN: %clangxx -fsycl %s -o %t.out
+// RUN: %timelimit %t.out > %t.txt 2>&1 || true
+// RUN: cat %t.txt | FileCheck %s
+// CHECK: timelimit:{{.*}}sycl!{{.*}}sycl::detail::enqueueImpKernel{{.*}}
+// CHECK: timelimit:{{.*}}sycl!{{.*}}sycl::handler::finalize{{.*}}
+// CHECK: timelimit:{{.*}}sycl!{{.*}}sycl::detail::queue_impl::finalizeHandler{{.*}}
+// CHECK: timelimit:{{.*}}sycl!{{.*}}sycl::detail::queue_impl::submit_impl{{.*}}
+
+#include <CL/sycl.hpp>
+
+using namespace cl::sycl;
+
+int main() {
+  queue Q;
+  // nd_range_error is generated due to 0-based local range.
+  Q.submit([&](handler &CGH) {
+     CGH.parallel_for_work_group<class f>(range<2>(5, 33), range<2>(1, 0),
+         [=](group<2>) {});
+  });
+  return 0;
+}

SYCL/lit.cfg.py

@@ -384,6 +384,13 @@
     else:
         lit_config.warning("Couldn't find pre-installed AOT device compiler " + aot_tool)
 
+# INTEL_CUSTOMIZATION
+if 'ICS_TESTDATA' in os.environ and platform.system() == "Windows":
+    config.available_features.add('timelimit')
+    # set _NT_SYMBOL_PATH to specify PDB files location
+    config.substitutions.append(('%timelimit', ' env _NT_SYMBOL_PATH='+config.dpcpp_root_dir+'/bin '+os.environ['ICS_TESTDATA']+'/mainline/CT-SpecialTests/opencl/tools/win.x64/bin/timelimit.exe'))
+# end INTEL_CUSTOMIZATION
+
 # Set timeout for test 1 min
 try:
     import psutil

config_sycl/pdb_sycl.info

@@ -0,0 +1 @@
+SYCL/PDB/sycl.cpp

llvm_test_suite_sycl.xml

@@ -542,6 +542,7 @@ Sources repo https://github.com/intel-innersource/applications.compilers.tests.l
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="matrix" testName="matrix_joint_matrix_uu_int8" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="onlinecompiler" testName="onlinecompiler_online_compiler_l0" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="onlinecompiler" testName="onlinecompiler_online_compiler_opencl" />
+    <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="pdb" testName="pdb_sycl" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="plugin" testName="plugin_enqueue_arg_order_buffer" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="plugin" testName="plugin_enqueue_arg_order_image" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="plugin" testName="plugin_interop_level_zero" />

llvm_test_suite_sycl_valgrind.xml

@@ -542,6 +542,7 @@ Sources repo https://github.com/intel-innersource/applications.compilers.tests.l
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="matrix" testName="matrix_joint_matrix_uu_int8" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="onlinecompiler" testName="onlinecompiler_online_compiler_l0" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="onlinecompiler" testName="onlinecompiler_online_compiler_opencl" />
+    <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="pdb" testName="pdb_sycl" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="plugin" testName="plugin_enqueue_arg_order_buffer" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="plugin" testName="plugin_enqueue_arg_order_image" />
     <test configFile="config_sycl/TEMPLATE_llvm_test_suite_sycl.xml" splitGroup="plugin" testName="plugin_interop_level_zero" />