Enable AOT tests back for A770 && BMG && WIN (#5049)

The main change is to not create the sycl device like this: `const
sycl::device sycl_device;` in global scope (doing this - led to a hang
on Windows).

---------

Signed-off-by: Anatoly Myachev <[email protected]>

Author: anmyachev

scripts/skiplist/a770/tools.txt

@@ -1,7 +0,0 @@
-python/test/unit/tools/test_aot.py::test_launcher_has_no_available_kernel[True]
-python/test/unit/tools/test_aot.py::test_launcher_has_no_available_kernel[False]
-python/test/unit/tools/test_aot.py::test_compile_link_matmul_no_specialization[True]
-python/test/unit/tools/test_aot.py::test_compile_link_matmul_no_specialization[False]
-python/test/unit/tools/test_aot.py::test_compile_link_matmul[True]
-python/test/unit/tools/test_aot.py::test_compile_link_matmul[False]
-python/test/unit/tools/test_aot.py::test_compile_link_autotune_matmul

scripts/skiplist/xe2/tools.txt

@@ -1,7 +0,0 @@
-python/test/unit/tools/test_aot.py::test_launcher_has_no_available_kernel[True]
-python/test/unit/tools/test_aot.py::test_launcher_has_no_available_kernel[False]
-python/test/unit/tools/test_aot.py::test_compile_link_matmul_no_specialization[True]
-python/test/unit/tools/test_aot.py::test_compile_link_matmul_no_specialization[False]
-python/test/unit/tools/test_aot.py::test_compile_link_matmul[True]
-python/test/unit/tools/test_aot.py::test_compile_link_matmul[False]
-python/test/unit/tools/test_aot.py::test_compile_link_autotune_matmul

third_party/intel/tools/intel/compile.cpp

@@ -29,18 +29,6 @@ static inline void gpuAssert(ze_result_t code, const char *file, int line) {{
 ze_module_handle_t {kernel_name}_mod = NULL;
 ze_kernel_handle_t {kernel_name}_func = NULL;
 unsigned char BIN_NAME[{bin_size}] = {{ {bin_data} }};
-// sycl globals
-const sycl::device sycl_device;
-const auto ctx =
-#if __SYCL_COMPILER_VERSION >= 20250604
-    sycl_device.get_platform().khr_get_default_context();
-#else
-    sycl_device.get_platform().ext_oneapi_get_default_context();
-#endif
-const auto l0_device =
-    sycl::get_native<sycl::backend::ext_oneapi_level_zero>(sycl_device);
-const auto l0_context =
-    sycl::get_native<sycl::backend::ext_oneapi_level_zero>(ctx);
 
 void unload_{kernel_name}(void) {{
     // Not implemeted
@@ -57,6 +45,17 @@ static ze_module_format_t get_module_format(const std::string& format_name) {{
 }}
 
 void load_{kernel_name}() {{
+    static sycl::device sycl_device;
+    static auto ctx =
+    #if __SYCL_COMPILER_VERSION >= 20250604
+        sycl_device.get_platform().khr_get_default_context();
+    #else
+        sycl_device.get_platform().ext_oneapi_get_default_context();
+    #endif
+    static auto l0_device =
+        sycl::get_native<sycl::backend::ext_oneapi_level_zero>(sycl_device);
+    static auto l0_context =
+        sycl::get_native<sycl::backend::ext_oneapi_level_zero>(ctx);
     uint8_t *binary_ptr = (uint8_t *)&BIN_NAME;
     size_t binary_size = {bin_size};
 
@@ -120,6 +119,7 @@ static inline void set_argument(sycl::handler &cgh, int index, const std::string
 }}
 
 int32_t {kernel_name}(sycl::queue &stream, {signature}) {{
+  const auto &ctx = stream.get_context();
   auto sycl_mod = sycl::make_kernel_bundle<sycl::backend::ext_oneapi_level_zero,
                                       sycl::bundle_state::executable>(
       {{{kernel_name}_mod, sycl::ext::oneapi::level_zero::ownership::transfer}}, ctx);