From 95718a0df1c07b825622b835af3fce3ff395c68c Mon Sep 17 00:00:00 2001 From: Andrey Alekseenko Date: Thu, 4 Nov 2021 18:37:42 +0100 Subject: [PATCH] SYCL: Avoid using no_init read accessor in rocFFT Currently, hipSYCL ends up ignoring no_init property in this case. But the SYCL standard does not permit such combination. --- src/gromacs/fft/gpu_3dfft_sycl_rocfft.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/src/gromacs/fft/gpu_3dfft_sycl_rocfft.cpp b/src/gromacs/fft/gpu_3dfft_sycl_rocfft.cpp index 8e59c7fe11..c5942dd807 100644 --- a/src/gromacs/fft/gpu_3dfft_sycl_rocfft.cpp +++ b/src/gromacs/fft/gpu_3dfft_sycl_rocfft.cpp @@ -409,7 +409,7 @@ void Gpu3dFft::ImplSyclRocfft::perform3dFft(gmx_fft_direction dir, CommandEvent* } // Enqueue the 3D FFT work impl_->queue_.submit([&](cl::sycl::handler& cgh) { - auto inputGridAccessor = inputGrid->get_access(cgh, cl::sycl::read_only, cl::sycl::no_init); + auto inputGridAccessor = inputGrid->get_access(cgh, cl::sycl::read_only); auto outputGridAccessor = outputGrid->get_access(cgh, cl::sycl::write_only, cl::sycl::no_init); // Use a hipSYCL custom operation to access the native buffers // needed to call rocFFT -- 2.22.0