// REQUIRES: aspect-ext_intel_legacy_image

// RUN: %{build} -o %t.out
// RUN: %{run} %t.out

// Test the image-specific printers of UR tracing.
//
// CHECK: <--- urMemImageCreate(
// CHECK-SAME:   image_desc w/h/d : 4 / 4 / 1  --  arrSz/row/slice : 0 / 64 / 256  --  num_mip_lvls/num_smpls/image_type : 0 / 0 / 4337
// CHECK: <--- urEnqueueMemBufferReadRect(
// CHECK-SAME:   ur_rect_offset_t x/y/z : 0/0/0
// CHECK-SAME:   ur_rect_region_t width/height/depth : 4/4/1

#include <sycl/accessor_image.hpp>
#include <sycl/detail/core.hpp>
#include <vector>

using namespace sycl;

int main() {
  const sycl::image_channel_order ChanOrder = sycl::image_channel_order::rgba;
  const sycl::image_channel_type ChanType = sycl::image_channel_type::fp32;

  constexpr auto SYCLWrite = sycl::access::mode::write;

  const sycl::range<2> ImgSize(4, 4);

  std::vector<sycl::float4> ImgHostData(ImgSize.size(), {1, 2, 3, 4});

  {
    sycl::image<2> Img(ImgHostData.data(), ChanOrder, ChanType, ImgSize);
    queue Q;

// legacy Images uses an API that is not supported in hip 4.x
#if HIP_VERSION_MAJOR >= 5
    Q.submit([&](sycl::handler &CGH) {
      auto ImgAcc = Img.get_access<sycl::float4, SYCLWrite>(CGH);

      CGH.single_task<class EmptyTask>([=]() {});
    });
#endif
  }
  return 0;
}