[SYCL][NFCI] Make sure that SYCL headers are self-contained (#13264)

Added a new set of auto-generated tests which check that each header in
`sycl/` directory is self-contained and therefore can be compiled
standalone.

Author: AlexeySachkov

sycl/include/CL/__spirv/spirv_vars.hpp

@@ -10,6 +10,7 @@
 
 #ifdef __SYCL_DEVICE_ONLY__
 
+#include <CL/__spirv/spirv_types.hpp>         // for __ocl_vec_t
 #include <sycl/detail/defines_elementary.hpp> // for __DPCPP_SYCL_EXTERNAL
 
 #include <cstddef> // for size_t

sycl/include/sycl/context.hpp

@@ -16,7 +16,6 @@
 #include <sycl/detail/info_desc_helpers.hpp>  // for is_context_info_desc
 #include <sycl/detail/owner_less_base.hpp>    // for OwnerLessBase
 #include <sycl/detail/pi.h>                   // for pi_native_handle
-#include <sycl/device.hpp>                    // for device
 #include <sycl/platform.hpp>                  // for platform
 #include <sycl/property_list.hpp>             // for property_list
 

sycl/include/sycl/detail/device_global_map.hpp

@@ -8,6 +8,8 @@
 
 #pragma once
 
+#include <sycl/detail/export.hpp>
+
 namespace sycl {
 inline namespace _V1 {
 namespace detail {

sycl/include/sycl/detail/group_sort_impl.hpp

@@ -12,6 +12,7 @@
 
 #ifdef __SYCL_DEVICE_ONLY__
 
+#include <sycl/builtins.hpp>
 #include <sycl/group_algorithm.hpp>
 #include <sycl/group_barrier.hpp>
 

sycl/include/sycl/detail/host_pipe_map.hpp

@@ -8,6 +8,8 @@
 
 #pragma once
 
+#include <sycl/detail/export.hpp>
+
 namespace sycl {
 inline namespace _V1 {
 namespace detail {

sycl/include/sycl/detail/kernel_properties.hpp

@@ -10,6 +10,7 @@
 
 #pragma once
 
+#include <sycl/detail/defines_elementary.hpp>
 #include <sycl/ext/oneapi/properties/property.hpp>
 #include <sycl/ext/oneapi/properties/property_value.hpp>
 

sycl/include/sycl/detail/reduction_forward.hpp

@@ -23,6 +23,7 @@
 
 namespace sycl {
 inline namespace _V1 {
+class handler;
 namespace detail {
 template <typename T, class BinaryOperation, int Dims, size_t Extent,
           bool ExplicitIdentity, typename RedOutVar>

sycl/include/sycl/detail/usm_impl.hpp

@@ -13,6 +13,8 @@
 
 namespace sycl {
 inline namespace _V1 {
+class device;
+
 namespace detail::usm {
 
 __SYCL_EXPORT void *alignedAlloc(size_t Alignment, size_t Bytes,

sycl/include/sycl/detail/vector_convert.hpp

@@ -55,6 +55,7 @@
 #pragma once
 
 #include <sycl/detail/generic_type_traits.hpp> // for is_sigeninteger, is_s...
+#include <sycl/exception.hpp>                  // for errc
 
 #ifndef __SYCL_DEVICE_ONLY__
 #include <cfenv> // for fesetround, fegetround

sycl/include/sycl/device_aspect_traits.hpp

@@ -8,7 +8,8 @@
 
 #pragma once
 
-#include "device_aspect_macros.hpp" // for aspect
+#include "device_aspect_macros.hpp" // for __SYCL_ALL_DEVICES_HAVE_* macro
+#include <sycl/aspects.hpp>         // for aspect
 
 #include <type_traits> // for bool_constant
 

sycl/include/sycl/ext/intel/esimd/detail/sycl_util.hpp

@@ -14,6 +14,7 @@
 /// @cond ESIMD_DETAIL
 
 #include <sycl/accessor.hpp>
+#include <sycl/ext/intel/esimd/detail/defines_elementary.hpp>
 
 namespace sycl {
 inline namespace _V1 {

sycl/include/sycl/ext/intel/esimd/math.hpp

@@ -17,6 +17,7 @@
 #include <sycl/ext/intel/esimd/detail/util.hpp>
 #include <sycl/ext/intel/esimd/simd.hpp>
 #include <sycl/ext/intel/esimd/simd_view.hpp>
+#include <sycl/ext/intel/experimental/esimd/detail/math_intrin.hpp>
 
 #include <cstdint>
 

sycl/include/sycl/ext/intel/esimd/memory_properties.hpp

@@ -8,6 +8,7 @@
 
 #pragma once
 
+#include <sycl/ext/intel/esimd/detail/defines_elementary.hpp>
 #include <sycl/ext/intel/experimental/fpga_utils.hpp>
 #include <sycl/ext/oneapi/experimental/common_annotated_properties/properties.hpp>
 #include <sycl/ext/oneapi/properties/properties.hpp>

sycl/include/sycl/ext/intel/esimd/xmx/dpas.hpp

@@ -14,6 +14,7 @@
 #include <sycl/ext/intel/esimd/detail/types.hpp>
 #include <sycl/ext/intel/esimd/xmx/common.hpp>
 #include <sycl/ext/intel/experimental/esimd/detail/math_intrin.hpp>
+#include <sycl/ext/intel/experimental/esimd/tfloat32.hpp>
 #include <sycl/ext/oneapi/bfloat16.hpp>
 
 namespace sycl {

sycl/include/sycl/ext/intel/experimental/detail/misc_intrin.hpp

@@ -13,6 +13,7 @@
 /// @cond SYCL_DETAIL
 
 #ifdef __SYCL_DEVICE_ONLY__
+#include <sycl/detail/defines_elementary.hpp>
 #define __SYCL_INTRIN __DPCPP_SYCL_EXTERNAL
 #else
 #define __SYCL_INTRIN inline

sycl/include/sycl/ext/intel/experimental/esimd/detail/math_intrin.hpp

@@ -15,6 +15,7 @@
 #include <sycl/ext/intel/esimd/detail/defines_elementary.hpp>
 #include <sycl/ext/intel/esimd/detail/math_intrin.hpp>
 #include <sycl/ext/intel/esimd/detail/types.hpp>
+#include <sycl/ext/intel/esimd/xmx/common.hpp>
 
 #define __ESIMD_raw_vec_t(T, SZ)                                               \
   sycl::ext::intel::esimd::detail::vector_type_t<                              \

sycl/include/sycl/ext/intel/experimental/esimd/detail/memory_intrin.hpp

@@ -14,6 +14,7 @@
 
 #include <sycl/ext/intel/esimd/detail/defines_elementary.hpp>
 #include <sycl/ext/intel/esimd/detail/memory_intrin.hpp>
+#include <sycl/ext/intel/experimental/esimd/common.hpp>
 
 // generic work-group split barrier
 __ESIMD_INTRIN void

sycl/include/sycl/ext/intel/experimental/grf_size_properties.hpp

@@ -9,6 +9,7 @@
 #pragma once
 
 #include <sycl/detail/kernel_properties.hpp>
+#include <sycl/ext/oneapi/properties/properties.hpp>
 #include <sycl/ext/oneapi/properties/property.hpp>
 #include <sycl/ext/oneapi/properties/property_value.hpp>
 

sycl/include/sycl/ext/intel/math.hpp

@@ -10,6 +10,8 @@
 
 #pragma once
 
+#include <cstdint>
+
 // _iml_half_internal is internal representation for fp16 type used in intel
 // math device library. The definition here should align with definition in
 // https://github.com/intel/llvm/blob/sycl/libdevice/imf_half.hpp

sycl/include/sycl/ext/intel/math/imf_fp_conversions.hpp

@@ -9,6 +9,8 @@
 //===----------------------------------------------------------------------===//
 
 #pragma once
+
+#include <sycl/ext/intel/math.hpp>
 #include <sycl/ext/oneapi/bfloat16.hpp>
 #include <sycl/half_type.hpp>
 

sycl/include/sycl/ext/intel/math/imf_half_trivial.hpp

@@ -9,6 +9,8 @@
 //===----------------------------------------------------------------------===//
 
 #pragma once
+
+#include <sycl/builtins.hpp>
 #include <sycl/half_type.hpp>
 
 namespace sycl {

sycl/include/sycl/ext/intel/math/imf_simd.hpp

@@ -10,6 +10,8 @@
 
 #pragma once
 
+#include <type_traits>
+
 extern "C" {
 unsigned int __imf_vabs2(unsigned int);
 unsigned int __imf_vabs4(unsigned int);

sycl/include/sycl/ext/intel/pipes.hpp

@@ -8,7 +8,8 @@
 
 #pragma once
 
-#include <sycl/exception.hpp> // for make_error_code, errc, exception
+#include <CL/__spirv/spirv_types.hpp> // for ConstantPipeStorage
+#include <sycl/exception.hpp>         // for make_error_code, errc, exception
 
 #include <stddef.h> // for size_t
 #include <stdint.h> // for int32_t
@@ -170,7 +171,7 @@ class kernel_readable_io_pipe {
   static constexpr int32_t m_Alignment = alignof(_dataT);
   static constexpr int32_t ID = _name::id;
 #ifdef __SYCL_DEVICE_ONLY__
-  static constexpr struct ConstantPipeStorage m_Storage
+  static constexpr ConstantPipeStorage m_Storage
       __attribute__((io_pipe_id(ID))) = {m_Size, m_Alignment, min_capacity};
 #endif // __SYCL_DEVICE_ONLY__
 };
@@ -221,7 +222,7 @@ class kernel_writeable_io_pipe {
   static constexpr int32_t m_Alignment = alignof(_dataT);
   static constexpr int32_t ID = _name::id;
 #ifdef __SYCL_DEVICE_ONLY__
-  static constexpr struct ConstantPipeStorage m_Storage
+  static constexpr ConstantPipeStorage m_Storage
       __attribute__((io_pipe_id(ID))) = {m_Size, m_Alignment, min_capacity};
 #endif // __SYCL_DEVICE_ONLY__
 };

sycl/include/sycl/ext/oneapi/accessor_property_list.hpp

@@ -234,6 +234,13 @@ class __SYCL_TYPE(accessor_property_list) accessor_property_list
                                   PropsT...>::value;
   }
 };
+
+namespace detail {
+template <typename T> struct is_accessor_property_list : std::false_type {};
+template <typename... Props>
+struct is_accessor_property_list<accessor_property_list<Props...>>
+    : std::true_type {};
+} // namespace detail
 } // namespace ext::oneapi
 
 } // namespace _V1

sycl/include/sycl/ext/oneapi/backend/hip.hpp

@@ -9,6 +9,7 @@
 #pragma once
 
 #include <sycl/backend.hpp>
+#include <sycl/detail/backend_traits_hip.hpp>
 
 namespace sycl {
 inline namespace _V1 {

sycl/include/sycl/ext/oneapi/bf16_storage_builtins.hpp

@@ -10,7 +10,7 @@
 
 #include <CL/__spirv/spirv_ops.hpp>
 #include <sycl/builtins.hpp>
-#include <sycl/detail/builtins.hpp>
+#include <sycl/detail/builtins/builtins.hpp>
 #include <sycl/detail/generic_type_lists.hpp>
 #include <sycl/detail/generic_type_traits.hpp>
 #include <sycl/detail/type_traits.hpp>

sycl/include/sycl/ext/oneapi/experimental/address_cast.hpp

@@ -7,6 +7,8 @@
 //===----------------------------------------------------------------------===//
 
 #pragma once
+
+#include <sycl/detail/spirv.hpp>
 #include <sycl/multi_ptr.hpp>
 
 namespace sycl {

sycl/include/sycl/ext/oneapi/experimental/alloca.hpp

@@ -8,9 +8,9 @@
 
 #pragma once
 
-#include "sycl/exception.hpp"
-#include "sycl/kernel_handler.hpp"
-#include "sycl/multi_ptr.hpp"
+#include <sycl/exception.hpp>
+#include <sycl/kernel_handler.hpp>
+#include <sycl/pointers.hpp>
 
 #ifdef __SYCL_DEVICE_ONLY__
 #include "sycl/aspects.hpp"

sycl/include/sycl/ext/oneapi/experimental/annotated_arg/annotated_arg.hpp

@@ -13,6 +13,7 @@
 #include <sycl/ext/oneapi/experimental/annotated_ptr/annotated_ptr_properties.hpp>
 #include <sycl/ext/oneapi/experimental/common_annotated_properties/properties.hpp>
 #include <sycl/ext/oneapi/properties/properties.hpp>
+#include <sycl/pointers.hpp>
 
 #include <cstddef>
 #include <type_traits>

sycl/include/sycl/ext/oneapi/experimental/annotated_ptr/annotated_ptr.hpp

@@ -17,6 +17,7 @@
 #include <sycl/ext/oneapi/properties/properties.hpp>
 #include <sycl/ext/oneapi/properties/property.hpp>
 #include <sycl/ext/oneapi/properties/property_value.hpp>
+#include <sycl/pointers.hpp>
 
 #include <cstddef>
 #include <string_view>

sycl/include/sycl/ext/oneapi/experimental/annotated_usm/alloc_base.hpp

@@ -10,9 +10,14 @@
 
 #include <sycl/ext/oneapi/experimental/annotated_ptr/annotated_ptr.hpp>
 #include <sycl/ext/oneapi/experimental/annotated_usm/alloc_util.hpp>
+#include <sycl/queue.hpp>
+#include <sycl/usm.hpp>
 
 namespace sycl {
 inline namespace _V1 {
+class device;
+class context;
+
 namespace ext {
 namespace oneapi {
 namespace experimental {
@@ -258,4 +263,4 @@ malloc_annotated(size_t count, const queue &syclQueue,
 } // namespace oneapi
 } // namespace ext
 } // namespace _V1
-} // namespace sycl
+} // namespace sycl

sycl/include/sycl/ext/oneapi/experimental/annotated_usm/alloc_util.hpp

@@ -9,7 +9,9 @@
 #pragma once
 
 #include <numeric>
+#include <sycl/ext/intel/experimental/usm_properties.hpp>
 #include <sycl/ext/oneapi/experimental/annotated_ptr/annotated_ptr.hpp>
+#include <sycl/property_list.hpp>
 
 namespace sycl {
 inline namespace _V1 {
@@ -245,4 +247,4 @@ inline size_t combine_align(size_t alignA, size_t alignB) {
 } // namespace oneapi
 } // namespace ext
 } // namespace _V1
-} // namespace sycl
+} // namespace sycl

sycl/include/sycl/ext/oneapi/experimental/annotated_usm/dealloc.hpp

@@ -9,6 +9,7 @@
 #pragma once
 
 #include <sycl/ext/oneapi/experimental/annotated_ptr/annotated_ptr.hpp>
+#include <sycl/usm.hpp>
 
 namespace sycl {
 inline namespace _V1 {
@@ -33,4 +34,4 @@ void free(annotated_ptr<T, propList> &ptr, const queue &syclQueue) {
 } // namespace oneapi
 } // namespace ext
 } // namespace _V1
-} // namespace sycl
+} // namespace sycl

sycl/include/sycl/ext/oneapi/experimental/cuda/barrier.hpp

@@ -8,6 +8,7 @@
 
 #pragma once
 
+#include <CL/__spirv/spirv_ops.hpp> // for __clc_BarrierInitialize
 #include <sycl/detail/pi.h>   // for PI_ERROR_INVALID_DEVICE
 #include <sycl/exception.hpp> // for runtime_error
 

sycl/include/sycl/ext/oneapi/experimental/fixed_size_group.hpp

@@ -12,6 +12,7 @@
 #include <sycl/detail/pi.h>            // for PI_ERROR_INVALID_DEVICE
 #include <sycl/detail/type_traits.hpp> // for is_fixed_size_group, is_group
 #include <sycl/exception.hpp>          // for runtime_error
+#include <sycl/ext/oneapi/experimental/non_uniform_groups.hpp>
 #include <sycl/ext/oneapi/sub_group_mask.hpp> // for sub_group_mask
 #include <sycl/id.hpp>                        // for id
 #include <sycl/memory_enums.hpp>              // for memory_scope

sycl/include/sycl/ext/oneapi/experimental/group_helpers_sorters.hpp

@@ -11,6 +11,7 @@
 #if (!defined(_HAS_STD_BYTE) || _HAS_STD_BYTE != 0)
 
 #include <sycl/aliases.hpp>             // for half
+#include <sycl/builtins.hpp>            // for min
 #include <sycl/detail/pi.h>             // for PI_ERROR_INVALID_DEVICE
 #include <sycl/exception.hpp>           // for sycl_category, exception
 #include <sycl/ext/oneapi/bfloat16.hpp> // for bfloat16

sycl/include/sycl/ext/oneapi/experimental/group_load_store.hpp

@@ -11,6 +11,7 @@
 #pragma once
 
 #include <sycl/ext/oneapi/properties/properties.hpp>
+#include <sycl/sycl_span.hpp>
 
 namespace sycl {
 inline namespace _V1 {

sycl/include/sycl/ext/oneapi/experimental/opportunistic_group.hpp

@@ -9,13 +9,16 @@
 #pragma once
 
 #include <sycl/aspects.hpp>
-#include <sycl/detail/pi.h>                   // for PI_ERROR_INVALID_DEVICE
-#include <sycl/detail/type_traits.hpp>        // for is_group, is_user_cons...
-#include <sycl/exception.hpp>                 // for runtime_error
+#include <sycl/detail/pi.h>            // for PI_ERROR_INVALID_DEVICE
+#include <sycl/detail/type_traits.hpp> // for is_group, is_user_cons...
+#include <sycl/exception.hpp>          // for runtime_error
+#include <sycl/ext/oneapi/experimental/non_uniform_groups.hpp>
+#include <sycl/ext/oneapi/free_function_queries.hpp> // for this_sub_group
 #include <sycl/ext/oneapi/sub_group_mask.hpp> // for sub_group_mask
 #include <sycl/id.hpp>                        // for id
 #include <sycl/memory_enums.hpp>              // for memory_scope
 #include <sycl/range.hpp>                     // for range
+#include <sycl/sub_group.hpp>
 
 #include <stdint.h>    // for uint32_t
 #include <type_traits> // for true_type