Github check-in test fixes

- ABI test failure fix
- Windows build fix

Author: dongkyunahn-intel

sycl/plugins/esimd_cpu/CMakeLists.txt

@@ -11,6 +11,26 @@ add_library(pi_esimd_cpu SHARED
   "pi_esimd_cpu.cpp"
 )
 
+if (MSVC)
+  # by defining __SYCL_BUILD_SYCL_DLL, we can use __declspec(dllexport)
+  # which are individually tagged for all pi* symbols in pi.h
+  target_compile_definitions(pi_esimd_cpu PRIVATE __SYCL_BUILD_SYCL_DLL)
+else()
+  # we set the visibility of all symbols 'hidden' by default.
+  # In pi.h file, we set exported symbols with visibility==default individually
+  target_compile_options(pi_esimd_cpu PUBLIC -fvisibility=hidden)
+
+  # This script file is used to allow exporting pi* symbols only.
+  # All other symbols are regarded as local (hidden)
+  set(linker_script "${CMAKE_CURRENT_SOURCE_DIR}/../ld-version-script.txt")
+
+  # Filter symbols based on the scope defined in the script file,
+  # and export pi* function symbols in the library.
+  target_link_libraries( pi_esimd_cpu
+    PRIVATE "-Wl,--version-script=${linker_script}"
+  )
+endif()
+
 add_dependencies(sycl-toolchain pi_esimd_cpu)
 
 add_dependencies(pi_esimd_cpu

sycl/source/detail/pi.cpp

@@ -65,7 +65,7 @@ void *getPluginOpaqueData(void *OpaqueDataParam) {
   return ReturnOpaqueData;
 }
 
-template void *getPluginOpaqueData<cl::sycl::backend::esimd_cpu>(void *);
+template __SYCL_EXPORT void *getPluginOpaqueData<cl::sycl::backend::esimd_cpu>(void *);
 
 namespace pi {
 
@@ -438,9 +438,9 @@ template <backend BE> const plugin &getPlugin() {
                       PI_INVALID_OPERATION);
 }
 
-template const plugin &getPlugin<backend::opencl>();
-template const plugin &getPlugin<backend::level_zero>();
-template const plugin &getPlugin<backend::esimd_cpu>();
+template __SYCL_EXPORT const plugin &getPlugin<backend::opencl>();
+template __SYCL_EXPORT const plugin &getPlugin<backend::level_zero>();
+template __SYCL_EXPORT const plugin &getPlugin<backend::esimd_cpu>();
 
 // Report error and no return (keeps compiler from printing warnings).
 // TODO: Probably change that to throw a catchable exception,

sycl/test/abi/sycl_symbols_linux.dump

@@ -3790,6 +3790,7 @@ _ZN2cl4sycl6detail18stringifyErrorCodeEi
 _ZN2cl4sycl6detail19convertChannelOrderE23_pi_image_channel_order
 _ZN2cl4sycl6detail19convertChannelOrderENS0_19image_channel_orderE
 _ZN2cl4sycl6detail19getImageElementSizeEhNS0_18image_channel_typeE
+_ZN2cl4sycl6detail19getPluginOpaqueDataILNS0_7backendE4EEEPvS4_
 _ZN2cl4sycl6detail19kernel_bundle_plain32set_specialization_constant_implEPKcPvm
 _ZN2cl4sycl6detail20associateWithHandlerERNS0_7handlerEPNS1_16AccessorBaseHostENS0_6access6targetE
 _ZN2cl4sycl6detail20getDeviceFromHandlerERNS0_7handlerE
@@ -3807,6 +3808,9 @@ _ZN2cl4sycl6detail28getPixelCoordNearestFiltModeENS0_3vecIfLi4EEENS0_15addressin
 _ZN2cl4sycl6detail2pi25contextSetExtendedDeleterERKNS0_7contextEPFvPvES6_
 _ZN2cl4sycl6detail2pi3dieEPKc
 _ZN2cl4sycl6detail2pi9assertionEbPKc
+_ZN2cl4sycl6detail2pi9getPluginILNS0_7backendE1EEERKNS1_6pluginEv
+_ZN2cl4sycl6detail2pi9getPluginILNS0_7backendE2EEERKNS1_6pluginEv
+_ZN2cl4sycl6detail2pi9getPluginILNS0_7backendE4EEERKNS1_6pluginEv
 _ZN2cl4sycl6detail6OSUtil10getDirNameB5cxx11EPKc
 _ZN2cl4sycl6detail6OSUtil11alignedFreeEPv
 _ZN2cl4sycl6detail6OSUtil12alignedAllocEmm