Почему на get_global_id в 2d возвращает странные значения?

Question

[cyberpunk9999]

Используя, например, фрагментный шейдер в GLSL получается градиент от начала до конца, однако в OpenCL получается какое - то безобразие. Хотя offset равен нулю по всем измерениям.
Итак, вот код kernel

__kernel void simple(__write_only image2d_t tex, int width, int height){
    const int x=get_global_id(0);      //Узнаем x координату
    const int y=get_global_id(1);      //y

    write_imagef (tex, (int2)(x, y), (float4)(x/(float)width,y/(float)height,0.0f,1.0f));   //Закрашиваем текстуру
}

И результат: