[SYCL] [FPGA] Create DSP control E2E emulator test (intel/llvm-test-suite#591)

Author: shuoniu-intel

SYCL/Basic/fpga_tests/fpga_dsp_control.cpp

@@ -0,0 +1,65 @@
+// RUN: %clangxx -fsycl -fintelfpga %s -o %t.out
+// RUN: %ACC_RUN_PLACEHOLDER %t.out
+//==---------- fpga_dsp_control.cpp - SYCL FPGA DSP control test -----------==//
+//
+// 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
+//
+//===----------------------------------------------------------------------===//
+#include <CL/sycl.hpp>
+#include <sycl/ext/intel/fpga_extensions.hpp>
+
+int test_dsp_control(cl::sycl::queue Queue) {
+  std::vector<float> input_data = {1.23f, 2.34f};
+  std::vector<float> output_data = {.0f, .0f};
+
+  {
+    cl::sycl::buffer input_buffer(input_data);
+    cl::sycl::buffer output_buffer(output_data);
+
+    Queue.submit([&](cl::sycl::handler &cgh) {
+      auto input_accessor =
+          input_buffer.get_access<cl::sycl::access::mode::read>(cgh);
+
+      auto output_accessor =
+          output_buffer.get_access<cl::sycl::access::mode::write>(cgh);
+
+      cgh.single_task<class kernel>([=] {
+        cl::sycl::ext::intel::math_dsp_control<
+            cl::sycl::ext::intel::Preference::DSP>(
+            [&] { output_accessor[0] = input_accessor[0] + 1.0f; });
+
+        cl::sycl::ext::intel::math_dsp_control<
+            cl::sycl::ext::intel::Preference::DSP,
+            cl::sycl::ext::intel::Propagate::Off>(
+            [&] { output_accessor[0] -= 1.0f; });
+
+        cl::sycl::ext::intel::math_dsp_control<
+            cl::sycl::ext::intel::Preference::Softlogic>(
+            [&] { output_accessor[1] = input_accessor[1] + 1.0f; });
+
+        cl::sycl::ext::intel::math_dsp_control<
+            cl::sycl::ext::intel::Preference::Softlogic,
+            cl::sycl::ext::intel::Propagate::Off>(
+            [&] { output_accessor[1] -= 1.0f; });
+      });
+    });
+  }
+
+  for (int i = 0; i < 2; i++) {
+    if (output_data[i] != input_data[i]) {
+      std::cout << "Unexpected read from output_data: " << output_data[i]
+                << ", v.s. expected " << input_data[i] << std::endl;
+
+      return -1;
+    }
+  }
+  return 0;
+}
+
+int main() {
+  cl::sycl::queue Queue{cl::sycl::ext::intel::fpga_emulator_selector{}};
+
+  return test_dsp_control(Queue);
+}

SYCL/Basic/fpga_tests/fpga_lsu.cpp

@@ -1,5 +1,5 @@
-// RUN: %clangxx -fsycl %s -o %t.out
-// RUNx: %ACC_RUN_PLACEHOLDER %t.out
+// RUN: %clangxx -fsycl -fintelfpga %s -o %t.out
+// RUN: %ACC_RUN_PLACEHOLDER %t.out
 //==----------------- fpga_lsu.cpp - SYCL FPGA LSU test --------------------==//
 //
 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
@@ -10,9 +10,6 @@
 #include <CL/sycl.hpp>
 #include <sycl/ext/intel/fpga_extensions.hpp>
 
-// TODO: run is disabled, since no support added in FPGA backend yet. Check
-// implementation correctness from CXX and SYCL languages perspective.
-
 int test_lsu(cl::sycl::queue Queue) {
   int output_data[2];
   for (size_t i = 0; i < 2; i++) {