Use OpenCL access qualifiers only for image objects

It seems I was overeager in adding those qualifiers to non-image buffers
as they are only defined by the standard in relation to image objects.
Adding the qualifiers to normal buffers causes no observable performance
difference on Nvidia targets and fails compilation when targeting AMD or
Intel.

1 files changed, 4 insertions, 4 deletions

diff --git a/template/particles.mako b/template/particles.mako
index cee3f4b..48191d9 100644
--- a/template/particles.mako
+++ b/template/particles.mako
@@ -1,7 +1,7 @@
-__kernel void update_particles(__global __read_only  float4* moments,
-                               __global __read_only  int*    material,
-                               __global __write_only float4* particles,
-                               __global __read_only  float4* init_particles,
+__kernel void update_particles(__global float4* moments,
+                               __global int*    material,
+                               __global float4* particles,
+                               __global float4* init_particles,
                                float aging)
 {
   const unsigned int pid = get_global_id(0);