block_opencl_kernel.cl 1.2 KB

123456789101112131415161718192021222324252627282930313233343536373839404142434445464748
  1. /* StarPU --- Runtime system for heterogeneous multicore architectures.
  2. *
  3. * Copyright (C) 2011-2012 Inria
  4. * Copyright (C) 2012,2015,2017 CNRS
  5. *
  6. * StarPU is free software; you can redistribute it and/or modify
  7. * it under the terms of the GNU Lesser General Public License as published by
  8. * the Free Software Foundation; either version 2.1 of the License, or (at
  9. * your option) any later version.
  10. *
  11. * StarPU is distributed in the hope that it will be useful, but
  12. * WITHOUT ANY WARRANTY; without even the implied warranty of
  13. * MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.
  14. *
  15. * See the GNU Lesser General Public License in COPYING.LGPL for more details.
  16. */
  17. __kernel void block_opencl(__global int *block,
  18. int nx, int ny, int nz,
  19. int ldy, int ldz,
  20. int factor, __global int *err)
  21. {
  22. const int id = get_global_id(0);
  23. if (id > 0)
  24. return;
  25. unsigned int i, j, k;
  26. int val = 0;
  27. for (k = 0; k < nz; k++)
  28. {
  29. for (j = 0; j < ny; j++)
  30. {
  31. for (i = 0; i < nx; i++)
  32. {
  33. if (block[(k*ldz)+(j*ldy)+i] != factor * val)
  34. {
  35. *err = 1;
  36. return;
  37. }
  38. else
  39. {
  40. block[(k*ldz)+(j*ldy)+i] *= -1;
  41. val++;
  42. }
  43. }
  44. }
  45. }
  46. }