[SYCL] Add STL wrapper for crtdbg.h and define _CrtDbgReport (#18213)

Wrapping around because want to define `_CrtDbgReport` before `crtdbg.h`
header is included. Defining variable templated `_CrtDbgReport`
overrides the use of variable argument `_CrtDbgReport` function, that
declared in `crtdbg.h`.

With variable argument `_CrtDbgReport`, `llvm-spirv` throws the
following error:
```
UnsupportedVarArgFunction: Variadic functions other than 'printf' are not supported in SPIR-V.
```
Fixes CMPLRLLVM-66787

---------

Signed-off-by: Agarwal, Udit <[email protected]>

Author: uditagarwal97

sycl/include/sycl/stl_wrappers/crtdbg.h

@@ -0,0 +1,41 @@
+//==---------------- Wrapper around crtdbg.h ------------------------------==//
+//
+// 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
+//
+//===----------------------------------------------------------------------===//
+
+// When std::array is used in device code, MSVC's STL uses _CrtDbgReport
+// function with variable arguments, when compiled in debug mode (-D_DEBUG
+// flag).
+
+// Variable argument functions are not supported in SPIR-V, and the compilation
+// fails with llvm-spirv error: UnsupportedVarArgFunction: Variadic functions
+// other than 'printf' are not supported in SPIR-V.
+
+// As a workaround, in this wrapper, we define our own variable templated
+// _CrtDbgReport which overrides the variable argument _CrtDbgReport function
+// declaration in crtdbg.h.
+
+// The variable templated _CrtDbgReport function has to be declared before the
+// crtdbg.h header is included, and that's why we have this STL wrapper instead
+// of declaring the _CrtDbgReport function in SYCL headers.
+
+#pragma once
+
+#if defined(__SYCL_DEVICE_ONLY__)
+template <typename... Ts> int _CrtDbgReport(Ts...) { return 0; }
+#endif
+
+#if defined(__has_include_next)
+// GCC/clang support go through this path.
+#include_next <crtdbg.h>
+#else
+// MSVC doesn't support "#include_next", so we have to be creative.
+// Our header is located in "stl_wrappers/crtdbg.h" so it won't be picked by the
+// following include. MSVC's installation, on the other hand, has the layout
+// where the following would result in the <crtdbg.h> we want. This is obviously
+// hacky, but the best we can do...
+#include <../ucrt/crtdbg.h>
+#endif

sycl/test/regression/std_array_vec_constructor.cpp

@@ -2,15 +2,12 @@
 // the constructor.
 // REQUIRES: windows
 
-// RUN: not %clangxx -O0 -fsycl -D_DEBUG -shared %s &> %t.compile.log
-// RUN: FileCheck %s -input-file=%t.compile.log
+// RUN: %clangxx -O0 -fsycl -D_DEBUG -shared %s -nostdlib -Xclang --dependent-lib=msvcrtd -fms-runtime-lib=dll_dbg
 
 #include <sycl/sycl.hpp>
 
 using namespace sycl::ext::oneapi::experimental;
 
-// CHECK: UnsupportedVarArgFunction: Variadic functions other than 'printf' are not supported in SPIR-V.
-// CHECK: clang{{.*}} error: llvm-spirv command failed with exit code 23{{.*}}
 auto Reproducer(sycl::queue q, sampled_image_handle imgHanlde) {
   return q.submit([&](sycl::handler &cg) {
     cg.parallel_for(