unsampled_image accessor mode

[orion160]

On SYCL 2020 reference get_access<DataT, Mode, Targ>. Mode needs to be read, or read_write. But on Intel 2024.0.2 I get a compilation error by an static assert.

// accessor.hpp
static_assert(AccessMode == access_mode::read || AccessMode == access_mode::write, "Access mode must be either read or write.");

https://registry.khronos.org/SYCL/specs/sycl-2020/html/sycl-2020.html#_unsampled_image_interface

Also what is image pitch, and why can I set it on a constructor?

#include <ImfArray.h>
#include <ImfRgbaFile.h>
#include <iostream>

#include <sycl/sycl.hpp>

int main(int argc, char **argv) {
  sycl::queue q{sycl::aspect_selector(sycl::aspect::fp16)};

  Imf::Rgba *pixels = nullptr;
  int width = -1;
  int height = -1;
  Imf::RgbaChannels channels;
  Imf::Compression compression;
  try {
    Imf::RgbaInputFile file("StillLife.exr");
    channels = file.channels();
    compression = file.compression();
    Imath::Box2i dw = file.dataWindow();
    width = dw.max.x - dw.min.x + 1;
    height = dw.max.y - dw.min.y + 1;
    pixels = new Imf::Rgba[width * height];

    file.setFrameBuffer(pixels, 1, width);
    file.readPixels(dw.min.y, dw.max.y);

  } catch (const std::exception &e) {
    std::cerr << "error reading image file StillLife.exr:" << e.what()
              << std::endl;
    return 1;
  }

  std::cout << "Channels: " << channels << '\n';
  std::cout << "Compression: " << compression << '\n';
  std::cout << "Image size: " << width << "x" << height << '\n';

  try {
    Imf::RgbaOutputFile file("out.exr", width, height, Imf::WRITE_RGBA);
    file.setFrameBuffer(pixels, 1, width);
    file.writePixels(height);
  } catch (const std::exception &e) {
    std::cerr << "Error writing image file out.exr:" << e.what() << std::endl;
    return 1;
  }

  {
    sycl::unsampled_image<2> img(pixels,
                                 sycl::image_format::r16b16g16a16_sfloat,
                                 sycl::range<2>(width, height));
    std::cout << "Byte size: " << img.byte_size() << '\n';
    std::cout << "width: " << img.get_range().get(0) << '\n';
    std::cout << "height: " << img.get_range().get(1) << '\n';
    std::cout << "size: " << img.size() << '\n';
    std::cout << "Pitch: " << img.get_pitch().get(0) << std::endl;
    q.submit([&](sycl::handler &h) {
      auto acc = img.get_access<sycl::half4, sycl::access_mode::read_write>(h);
    });
  }

  delete[] pixels;

  return 0;
}