[SYCL] Remove some OSUtil::* funcs from ABI (#20694)

Removing unused `OSUtil::*` ABI entry points since we are in the
breaking window.
Co-authored-by: Steffen Larsen <steffen.larsen@intel.com>

Author: againull

sycl/include/sycl/detail/os_util.hpp

@@ -44,21 +44,9 @@ namespace detail {
 
 /// Groups the OS-dependent services.
 class __SYCL_EXPORT OSUtil {
-#if !defined(__INTEL_PREVIEW_BREAKING_CHANGES)
-#ifdef _WIN32
-  // Access control is part of the mangling on Windows, have to preserve this
-  // for backward ABI compatibility.
-public:
-#endif
-  /// Returns a directory component of a path.
-  static std::string getDirName(const char *Path);
-#endif
-
 public:
   /// Returns an absolute path to a directory where the object was found.
-#if defined(__INTEL_PREVIEW_BREAKING_CHANGES)
   __SYCL_DLL_LOCAL
-#endif
   static std::string getCurrentDSODir();
 
 #ifdef __SYCL_RT_OS_WINDOWS

sycl/source/detail/os_util.cpp

@@ -58,12 +58,7 @@ namespace sycl {
 inline namespace _V1 {
 namespace detail {
 
-#if defined(__INTEL_PREVIEW_BREAKING_CHANGES)
-[[maybe_unused]] static std::string getDirName(const char *Path)
-#else
-std::string OSUtil::getDirName(const char *Path)
-#endif
-{
+[[maybe_unused]] static std::string getDirName(const char *Path) {
   return fs::path(Path).parent_path().string();
 }
 

sycl/test/abi/sycl_abi_neutrality_test.cpp

@@ -22,10 +22,6 @@
 // https://github.com/intel/llvm/pull/16178
 // CHECK:_ZN4sycl3_V13ext5intel12experimental9pipe_base13get_pipe_nameB5cxx11EPKv
 //
-// https://github.com/intel/llvm/pull/16177
-// CHECK:_ZN4sycl3_V16detail6OSUtil10getDirNameB5cxx11EPKc
-// CHECK:_ZN4sycl3_V16detail6OSUtil16getCurrentDSODirB5cxx11Ev
-//
 // https://github.com/intel/llvm/pull/16176
 // CHECK:_ZN4sycl3_V16opencl13has_extensionERKNS0_6deviceERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE
 // CHECK:_ZN4sycl3_V16opencl13has_extensionERKNS0_8platformERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE

sycl/test/abi/sycl_symbols_linux.dump

@@ -3356,11 +3356,9 @@ _ZN4sycl3_V16detail35sampledImageConstructorNotificationEPvS2_RKSt8optionalINS0_
 _ZN4sycl3_V16detail36addHostUnsampledImageAccessorAndWaitEPNS1_30UnsampledImageAccessorImplHostE
 _ZN4sycl3_V16detail36get_empty_interop_kernel_bundle_implERKNS0_7contextERKSt6vectorINS0_6deviceESaIS6_EE
 _ZN4sycl3_V16detail37unsampledImageConstructorNotificationEPvS2_RKSt8optionalINS0_12image_targetEENS0_6access4modeEPKvjRKNS1_13code_locationE
-_ZN4sycl3_V16detail6OSUtil10getDirNameB5cxx11EPKc
 _ZN4sycl3_V16detail6OSUtil11alignedFreeEPv
 _ZN4sycl3_V16detail6OSUtil12alignedAllocEmm
 _ZN4sycl3_V16detail6OSUtil12getOSMemSizeEv
-_ZN4sycl3_V16detail6OSUtil16getCurrentDSODirB5cxx11Ev
 _ZN4sycl3_V16detail6OSUtil7makeDirEPKc
 _ZN4sycl3_V16detail9join_implERKSt6vectorISt10shared_ptrINS1_18kernel_bundle_implEESaIS5_EENS0_12bundle_stateE
 _ZN4sycl3_V16detail9link_implEPKNS0_13kernel_bundleILNS0_12bundle_stateE1EEEmRKSt6vectorINS0_6deviceESaIS8_EEb

sycl/test/abi/sycl_symbols_windows.dump

@@ -4033,7 +4033,6 @@
 ?getDeviceBackend@handler@_V1@sycl@@AEBA?AW4backend@23@XZ
 ?getDeviceFromHandler@detail@_V1@sycl@@YA?AVdevice@23@AEAVhandler@23@@Z
 ?getDeviceKernelInfo@detail@_V1@sycl@@YAAEAVDeviceKernelInfo@123@AEBUCompileTimeKernelInfoTy@compile_time_kernel_info_v1@123@@Z
-?getDirName@OSUtil@detail@_V1@sycl@@SA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@PEBD@Z
 ?getElemSize@AccessorBaseHost@detail@_V1@sycl@@QEBAIXZ
 ?getElementSize@LocalAccessorBaseHost@detail@_V1@sycl@@QEAAHXZ
 ?getElementSize@SampledImageAccessorBaseHost@detail@_V1@sycl@@QEBAHXZ

sycl/unittests/misc/OsUtils.cpp

@@ -54,12 +54,10 @@ bool isSameDir(const char* LHS, const char* RHS) {
 class OsUtilsTest : public ::testing::Test {
 };
 
-// This test fails with preview breaking changes enabled.
-// Failure tracker: https://github.com/intel/llvm/issues/19626
-#ifndef __INTEL_PREVIEW_BREAKING_CHANGES
 TEST_F(OsUtilsTest, getCurrentDSODir) {
+  // Failure tracker: https://github.com/intel/llvm/issues/19626
+  GTEST_SKIP() << "Skipping test due to failure tracked in issue #19626";
   std::string DSODir = sycl::detail::OSUtil::getCurrentDSODir();
   ASSERT_TRUE(isSameDir(DSODir.c_str(), SYCL_LIB_DIR)) <<
       "expected: " << SYCL_LIB_DIR << ", got: " << DSODir;
 }
-#endif