[SYCL] Use public interfaces in function_pointer.hpp

This patch is a part of effort to decouple SYCL Runtime library
interface from its actual implementation. The goal is to improve
SYCL ABI/API compatibility between different versions of library.

Two helper functions were introduced to eliminate calls to _impl
classes. This caused 3 tests fail. 2 tests were found to use
internal APIs. Missing include clauses were added to workaround
those fails. A more robust solution will be provided in separate
patches.

Signed-off-by: Alexander Batashev <[email protected]>

Author: Alexander Batashev

sycl/include/CL/sycl/intel/function_pointer.hpp

@@ -8,7 +8,6 @@
 
 #pragma once
 
-#include <CL/sycl/detail/program_impl.hpp>
 #include <CL/sycl/device.hpp>
 #include <CL/sycl/program.hpp>
 #include <CL/sycl/stl.hpp>
@@ -17,6 +16,11 @@
 
 __SYCL_INLINE namespace cl {
 namespace sycl {
+namespace detail {
+// Helper functions to avoid calls to implementation detail methods.
+pi_device getRawDevice(device &D);
+pi_program getRawProgram(program &P);
+} // namespace detail
 namespace intel {
 
 // This is a preview extension implementation, intended to provide early access
@@ -27,7 +31,7 @@ namespace intel {
 // products. If you are interested in using this feature in your software
 // product, please let us know!
 
-using device_func_ptr_holder_t = cl::sycl::cl_ulong;
+using device_func_ptr_holder_t = cl_ulong;
 
 /// \brief this function performs a cast from device_func_ptr_holder_t type
 /// to the provided function pointer type.
@@ -82,9 +86,7 @@ device_func_ptr_holder_t get_device_func_ptr(FuncType F, const char *FuncName,
   // FIXME: return value must be checked here, but since we cannot yet check
   // if corresponding extension is supported, let's silently ignore it here.
   PI_CALL(piextGetDeviceFunctionPointer)(
-      detail::pi::cast<pi_device>(detail::getSyclObjImpl(D)->getHandleRef()),
-      detail::pi::cast<pi_program>(detail::getSyclObjImpl(P)->getHandleRef()),
-      FuncName, &FPtr);
+      detail::getRawDevice(D), detail::getRawProgram(P), FuncName, &FPtr);
 
   return FPtr;
 }

sycl/source/CMakeLists.txt

@@ -88,6 +88,7 @@ set(SYCL_SOURCES
     "event.cpp"
     "exception.cpp"
     "exception_list.cpp"
+    "function_pointer.cpp"
     "half_type.cpp"
     "handler.cpp"
     "kernel.cpp"

sycl/source/function_pointer.cpp

@@ -0,0 +1,25 @@
+//==----------- function_pointer.cpp --- SYCL Function pointers ------------==//
+//
+// 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/detail/program_impl.hpp>
+#include <CL/sycl/intel/function_pointer.hpp>
+
+__SYCL_INLINE namespace cl {
+  namespace sycl {
+  namespace detail {
+  pi_device getRawDevice(device &D) {
+    return detail::pi::cast<pi_device>(
+        detail::getSyclObjImpl(D)->getHandleRef());
+  }
+  pi_program getRawProgram(program &P) {
+    return detail::pi::cast<pi_program>(
+        detail::getSyclObjImpl(P)->getHandleRef());
+  }
+  } // namespace detail
+  } // namespace sycl
+}

sycl/test/basic_tests/image_api.cpp

@@ -7,6 +7,9 @@
 // RUN: %ACC_RUN_PLACEHOLDER %t1.out
 
 #include <CL/sycl.hpp>
+// FIXME do not use internal methods in tests.
+#include <CL/sycl/detail/cg.hpp>
+#include <CL/sycl/detail/kernel_impl.hpp>
 
 #include <algorithm>
 #include <array>

sycl/test/kernel-and-program/cache.cpp

@@ -9,6 +9,8 @@
 //===----------------------------------------------------------------------===//
 
 #include <CL/sycl.hpp>
+// FIXME do not use internal methods in tests.
+#include <CL/sycl/detail/program_impl.hpp>
 
 namespace RT = cl::sycl::RT;
 namespace detail = cl::sycl::detail;

sycl/test/sub_group/common_ocl.cpp

@@ -16,7 +16,9 @@
 #include "helper.hpp"
 #include <CL/sycl.hpp>
 #include <cstring>
+#include <fstream>
 #include <iostream>
+
 using namespace cl::sycl;
 struct Data {
   unsigned int local_id;