[SYCL] Tests for the Plugin Interface tracing

SYCL/Tracing/buffer_printers.cpp

@@ -0,0 +1,55 @@
+// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple  %s -o %t.out
+// RUN: env SYCL_PI_TRACE=2 %GPU_RUN_PLACEHOLDER %t.out %GPU_CHECK_PLACEHOLDER
+// RUN: env SYCL_PI_TRACE=2 %CPU_RUN_PLACEHOLDER %t.out %CPU_CHECK_PLACEHOLDER
+// RUN: env SYCL_PI_TRACE=2 %ACC_RUN_PLACEHOLDER %t.out %ACC_CHECK_PLACEHOLDER
+
+#include <CL/sycl.hpp>
+#include <vector>
+
+// Test image-specific printers of the Plugin Interace
+//
+//CHECK: ---> piEnqueueMemBufferCopyRect(
+//CHECK:   pi_buff_rect_offset x_bytes/y/z : 64/5/0
+//CHECK:   pi_buff_rect_offset x_bytes/y/z : 0/0/0
+//CHECK:   pi_buff_rect_region width_bytes/height/depth : 64/5/1
+//CHECK:   pi_buff_rect_region width_bytes/height/depth : 64/5/1
+
+using namespace cl::sycl;
+
+int main() {
+  constexpr unsigned Width = 16;
+  constexpr unsigned Height = 5;
+  constexpr unsigned Total = Width * Height;
+
+  std::vector<int> SrcData(Total * 4, 7);
+  std::vector<int> DstData(Total, 0);
+
+  queue Queue;
+  {
+    buffer<int, 2> SrcBuffer(SrcData.data(), range<2>(Height * 2, Width * 2));
+    buffer<int, 2> DstBuffer(DstData.data(), range<2>(Height, Width));
+
+    Queue.submit([&](handler &CGH) {
+      auto Read = SrcBuffer.get_access<access::mode::read>(
+          CGH, range<2>(Height, Width), id(Height, Width));
+      auto Write = DstBuffer.get_access<access::mode::write>(CGH);
+      CGH.copy(Read, Write);
+    });
+  }
+
+  // CHECK: ---> piMemBufferPartition(
+  // CHECK:   pi_buffer_region origin/size : 128/32
+
+  constexpr unsigned Size = 64;
+  std::vector<int> Data(Size);
+  {
+    cl::sycl::buffer<int, 1> Buf(Data.data(), Size);
+    cl::sycl::buffer<int, 1> SubBuf(Buf, Size / 2, 8);
+
+    Queue.submit([&](cl::sycl::handler &CGH) {
+      auto Acc = SubBuf.get_access<cl::sycl::access::mode::write>(CGH);
+      CGH.single_task<class empty_task>([=]() {});
+    });
+  }
+  return 0;
+}

SYCL/Tracing/image_printers.cpp

@@ -0,0 +1,38 @@
+// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
+// RUN: %CPU_RUN_PLACEHOLDER %t.out
+// RUN: %GPU_RUN_PLACEHOLDER %t.out
+
+// Test image-specific printers of the Plugin Interace
+//
+// CHECK: ---> piMemImageCreate(
+// CHECK:   image_desc w/h/d : 4 / 4 / 1  --  arrSz/row/slice : 0 / 64 / 256  --  num_mip_lvls/num_smpls/image_type : 0 / 0 / 4337
+// CHECK: ---> piEnqueueMemImageRead(
+// CHECK:   pi_image_offset x/y/z : 0/0/0
+// CHECK:   pi_image_region width/height/depth : 4/4/1
+
+#include <CL/sycl.hpp>
+#include <vector>
+
+using namespace sycl;
+
+int main() {
+  const sycl::image_channel_order ChanOrder = sycl::image_channel_order::rgba;
+  const sycl::image_channel_type ChanType = sycl::image_channel_type::fp32;
+
+  constexpr auto SYCLWrite = sycl::access::mode::write;
+
+  const sycl::range<2> ImgSize(4, 4);
+
+  std::vector<sycl::float4> ImgHostData(ImgSize.size(), {1, 2, 3, 4});
+
+  {
+    sycl::image<2> Img(ImgHostData.data(), ChanOrder, ChanType, ImgSize);
+    queue Q;
+    Q.submit([&](sycl::handler &CGH) {
+      auto ImgAcc = Img.get_access<sycl::float4, SYCLWrite>(CGH);
+
+      CGH.single_task<class EmptyTask>([=]() {});
+    });
+  }
+  return 0;
+}

SYCL/Tracing/pi_tracing_test.cpp

@@ -0,0 +1,57 @@
+// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
+// RUN: env SYCL_PI_TRACE=-1 %CPU_RUN_PLACEHOLDER %t.out %CPU_CHECK_PLACEHOLDER
+// RUN: env SYCL_PI_TRACE=-1 %GPU_RUN_PLACEHOLDER %t.out %GPU_CHECK_PLACEHOLDER
+// RUN: env SYCL_PI_TRACE=-1 %ACC_RUN_PLACEHOLDER %t.out %ACC_CHECK_PLACEHOLDER
+
+// Test tracing of the Plugin Interface
+
+// CHECK: ---> piPlatformGetInfo(
+// CHECK:  pi_platform : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK:  <char * > : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK:  <nullptr>
+// CHECK: ---> piMemBufferCreate(
+// CHECK-NEXT:  <unknown> : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK-NEXT:  <unknown> : 1
+// CHECK-NEXT:  <unknown> : 40
+// CHECK-NEXT:  <unknown> : 0
+// CHECK-NEXT:  <unknown> : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK:  <nullptr>
+// CHECK-NEXT: ) ---> 	pi_result : PI_SUCCESS
+// CHECK-NEXT: [out]void * : {{0+}}
+// CHECK-NEXT: [out]pi_mem * : {{0[xX]?[0-9a-fA-F]*}}[ {{0[xX]?[0-9a-fA-F]*}}
+// CHECK: ---> piKernelCreate(
+// CHECK:  <const char *>: {{.*}}
+// CHECK: ---> piEnqueueKernelLaunch(
+// CHECK-NEXT:  <unknown> : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK-NEXT:  <unknown> : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK-NEXT:  <unknown> : 1
+// CHECK-NEXT:  <unknown> : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK-NEXT:  <unknown> : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK-NEXT:  <unknown> : 0
+// CHECK-NEXT:  <unknown> : 0
+// CHECK-NEXT:  pi_event * : {{0+}}[ nullptr ]
+// CHECK-NEXT:  pi_event * : {{0[xX]?[0-9a-fA-F]*}}[ {{0+}} ... ]
+// CHECK-NEXT: ) ---> 	pi_result : PI_SUCCESS
+// CHECK-NEXT: [out]pi_event * : {{0+}}[ nullptr ]
+// CHECK-NEXT: [out]pi_event * : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK-SAME: [ {{0[xX]?[0-9a-fA-F]*}} ... ]
+//
+// CHECK: ---> piEventsWait(
+// CHECK-NEXT:  <unknown> : 1
+// CHECK-NEXT:  const pi_event * : {{0[xX]?[0-9a-fA-F]*}}
+// CHECK-SAME:  [ {{0[xX]?[0-9a-fA-F]*}} ... ]
+// CHECK-NEXT: ) ---> 	pi_result : PI_SUCCESS
+
+#include <CL/sycl.hpp>
+int main() {
+  cl::sycl::queue Queue;
+  cl::sycl::buffer<int, 1> Buf(10);
+  Queue.submit([&](cl::sycl::handler &cgh) {
+    auto Acc = Buf.template get_access<cl::sycl::access::mode::read_write>(cgh);
+
+    cgh.parallel_for<class CheckTraces>(
+        10, [=](cl::sycl::id<1> ID) { Acc[ID] = 5; });
+  });
+  Queue.wait();
+  return 0;
+}