[SYCL] Throw exception when device does not support queries in sycl_ext_intel_device_info (#14788)

This PR implements specializations of `get_device_info` function for the
queries defined in
[sycl_ext_intel_device_info](https://github.com/intel/llvm/blob/sycl/sycl/doc/extensions/supported/sycl_ext_intel_device_info.md)
so that when a device does not support the corresponding aspect for a
query, an exception is thrown with error code set to
`errc::feature_not_supported` as stipulated in the extension spec.

Author: lbushi25

sycl/source/detail/device_info.hpp

@@ -1273,16 +1273,161 @@ template <typename Param>
 typename Param::return_type get_device_info(const DeviceImplPtr &Dev) {
   static_assert(is_device_info_desc<Param>::value,
                 "Invalid device information descriptor");
-  if (std::is_same<Param,
-                   sycl::_V1::ext::intel::info::device::free_memory>::value) {
-    if (!Dev->has(aspect::ext_intel_free_memory))
-      throw exception(
-          make_error_code(errc::invalid),
-          "The device does not have the ext_intel_free_memory aspect");
-  }
   return get_device_info_impl<typename Param::return_type, Param>::get(Dev);
 }
 
+template <>
+inline ext::intel::info::device::device_id::return_type
+get_device_info<ext::intel::info::device::device_id>(const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_device_id))
+    throw exception(make_error_code(errc::feature_not_supported),
+                    "The device does not have the ext_intel_device_id aspect");
+  using Param = ext::intel::info::device::device_id;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::uuid::return_type
+get_device_info<ext::intel::info::device::uuid>(const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_device_info_uuid))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_device_info_uuid aspect");
+  using Param = ext::intel::info::device::uuid;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::pci_address::return_type
+get_device_info<ext::intel::info::device::pci_address>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_pci_address))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_pci_address aspect");
+  using Param = ext::intel::info::device::pci_address;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::gpu_eu_simd_width::return_type
+get_device_info<ext::intel::info::device::gpu_eu_simd_width>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_gpu_eu_simd_width))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_gpu_eu_simd_width aspect");
+  using Param = ext::intel::info::device::gpu_eu_simd_width;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::gpu_eu_count::return_type
+get_device_info<ext::intel::info::device::gpu_eu_count>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_gpu_eu_count))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_gpu_eu_count aspect");
+  using Param = ext::intel::info::device::gpu_eu_count;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::gpu_slices::return_type
+get_device_info<ext::intel::info::device::gpu_slices>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_gpu_slices))
+    throw exception(make_error_code(errc::feature_not_supported),
+                    "The device does not have the ext_intel_gpu_slices aspect");
+  using Param = ext::intel::info::device::gpu_slices;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::gpu_subslices_per_slice::return_type
+get_device_info<ext::intel::info::device::gpu_subslices_per_slice>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_gpu_subslices_per_slice))
+    throw exception(make_error_code(errc::feature_not_supported),
+                    "The device does not have the "
+                    "ext_intel_gpu_subslices_per_slice aspect");
+  using Param = ext::intel::info::device::gpu_subslices_per_slice;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::gpu_eu_count_per_subslice::return_type
+get_device_info<ext::intel::info::device::gpu_eu_count_per_subslice>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_gpu_eu_count_per_subslice))
+    throw exception(make_error_code(errc::feature_not_supported),
+                    "The device does not have the "
+                    "ext_intel_gpu_eu_count_per_subslice aspect");
+  using Param = ext::intel::info::device::gpu_eu_count_per_subslice;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::gpu_hw_threads_per_eu::return_type
+get_device_info<ext::intel::info::device::gpu_hw_threads_per_eu>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_gpu_hw_threads_per_eu))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_gpu_hw_threads_per_eu aspect");
+  using Param = ext::intel::info::device::gpu_hw_threads_per_eu;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::max_mem_bandwidth::return_type
+get_device_info<ext::intel::info::device::max_mem_bandwidth>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_max_mem_bandwidth))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_max_mem_bandwidth aspect");
+  using Param = ext::intel::info::device::max_mem_bandwidth;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::free_memory::return_type
+get_device_info<ext::intel::info::device::free_memory>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_free_memory))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_free_memory aspect");
+  using Param = ext::intel::info::device::free_memory;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::memory_clock_rate::return_type
+get_device_info<ext::intel::info::device::memory_clock_rate>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_memory_clock_rate))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_memory_clock_rate aspect");
+  using Param = ext::intel::info::device::memory_clock_rate;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
+template <>
+inline ext::intel::info::device::memory_bus_width::return_type
+get_device_info<ext::intel::info::device::memory_bus_width>(
+    const DeviceImplPtr &Dev) {
+  if (!Dev->has(aspect::ext_intel_memory_bus_width))
+    throw exception(
+        make_error_code(errc::feature_not_supported),
+        "The device does not have the ext_intel_memory_bus_width aspect");
+  using Param = ext::intel::info::device::memory_bus_width;
+  return get_device_info_impl<Param::return_type, Param>::get(Dev);
+}
+
 // Returns the list of all progress guarantees that can be requested for
 // work_groups from the coordination level of root_group when using the device
 // given by Dev. First it calls getProgressGuarantee to get the strongest

sycl/test-e2e/Basic/get_info_aspect.cpp

@@ -17,7 +17,7 @@ int main() {
     sycl::device d(sycl::default_selector_v);
     size_t mem_free = d.get_info<sycl::ext::intel::info::device::free_memory>();
   } catch (const sycl::exception &e) {
-    assert(e.code() == sycl::errc::invalid);
+    assert(e.code() == sycl::errc::feature_not_supported);
     std::cout << "Expected exception encountered: " << e.what() << std::endl;
     failed = false;
   }