block_opencl_kernel.cl 1.2 KB

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