OpenGL/OpenCL kernel wird nicht ausgefürt

[Daniel A. (daniel-a)]

Ich habe schon einiges mit OpenGL gemacht, und wollte jetzt etwas mit 
OpenCL ausprobieren.
Meine Idee war es, das Doublebuffering auszuschalten, und dieses mit 
einem Renderbuffer-Object und einem Framebuffer-Object zu simulieren, um 
den Renderbuffer in OpenCL nutzen zu können.
Es scheint alles bestens zu funktionieren, mit gDEBugger und AMD CodeX 
konnte ich sehen, dass alle OpenGL und OpenCL Funktionen in der 
erwarteten Reihenfolge ausgeführt werden, es gibt keine Fehlermeldungen, 
Compilerflags -Wall -Wextra -pedantic und -Werror sind gesetzt, aber das 
Fenster ist grün statt rot.

Der Kernel scheint entweder nicht ausgeführt zu werden, oder aber nichts 
zu tun.

Ich kann den Fehler einfach nicht finden. Könnte mir bitte jemand einen 
hinweis geben?

Einige infos zu meinem PC:

  gcc (Ubuntu 4.9.2-0ubuntu1~14.04) 4.9.2

  CL_DEVICE_NAME:        GeForce GT 650M
  CL_DEVICE_VENDOR:      NVIDIA Corporation
  CL_DEVICE_VERSION:     OpenCL 1.1 CUDA
  CL_DEVICE_TYPE:        CL_DEVICE_TYPE_GPU
  CL_DRIVER_VERSION:     331.38
  CL_DEVICE_PROFILE:     FULL_PROFILE
  CL_DEVICE_MAX_COMPUTE_UNITS:   2
  CL_DEVICE_MAX_CLOCK_FREQUENCY:         835
  CL_DEVICE_MEM_BASE_ADDR_ALIGN:         4096
  CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE:    128

main loop (verkleinert, vollständige Version ist im Anhang):

  while(1){

    size_t fb_size[] = {
      w->winWidth,w->winHeight,0
    };

    glBindFramebuffer(GL_DRAW_FRAMEBUFFER, w->buffer.gl_frame);
    glClear(GL_COLOR_BUFFER_BIT);
    glBindFramebuffer(GL_DRAW_FRAMEBUFFER, 0 );


    glFinish();
    clEnqueueAcquireGLObjects(w->clCommandQueue,1,&w->buffer.cl_color,0,0,0);


    clSetKernelArg(w->kernel.raytracer_drawScene, 0, sizeof(cl_mem), &w->buffer.cl_color);
    clEnqueueNDRangeKernel( w->clCommandQueue, w->kernel.raytracer_drawScene, 1, 0, fb_size, 0, 0, 0, 0 );


    clEnqueueReleaseGLObjects(w->clCommandQueue,1,&w->buffer.cl_color,0,0,0);
    clFinish(w->clCommandQueue);


    glBlitFramebuffer(0,0,w->winWidth, w->winHeight,0,0,w->winWidth, w->winHeight,GL_COLOR_BUFFER_BIT,GL_NEAREST);

  }

Der OpenCL kernel:

kernel void raytracer_drawScene(global write_only image2d_t fb){

  const int2 xy = {
    get_global_id(0),
    get_global_id(1)
  };

  const uint4 color = { 255,0, 0, 127 };

  write_imageui(fb, xy, color);

}

[Daniel A. (daniel-a)]

Ich konnte den Fehler immernochnicht finden, und würde mich sehr über 
eine Antwort freuen.

Da die Frage womöglich nicht ideal für ein Mikrocontroller forum ist, 
bin ich auch sehr an Erfahrungsberichten über foren mit Spezialisierung 
auf OpenCL und OpenGL interessiert.

[mar IO (Gast)]

Kann dir leider ned weiterhelfen. Auch Foren kenn ich dazu keine, aber 
einfach mal den Standard ausprobieren:
- OpenCL ist von der Khronos Group. Einfach mal da nach einem Forum 
suchen (gibt es, hab gerade gekuckt).
- Bei Stackoverflow sind sicherlich auch Leute unterwegs, die davon 
Ahnung haben (OpenCL-Tag hat z.Z. 2615 Threads).

[Eric B. (beric)]

Daniel A. schrieb:
> const uint4 color = { 255,0, 0, 127 };

Was passiert wenn du da mal
{0, 255, 0, 127 } reinschreibst? Immer noch grün?

[Daniel A. (daniel-a)]

mar IO schrieb:
> Auch Foren kenn ich dazu keine, aber
> einfach mal den Standard ausprobieren

Trotzdem Danke, ich denke dass werde ich tun.

Eric B. schrieb:
> Was passiert wenn du da mal
> {0, 255, 0, 127 } reinschreibst? Immer noch grün?

Ja. Das grün kommt von glClear(GL_COLOR_BUFFER_BIT)
Mit glClearColor hab ich grün angegeben. Es sollte danach aber nach 
clEnqueueNDRangeKernel mit Rot übermalt werden. Auskommentieren von 
glClearColor führt dazu, dass der zufällige initiale Inhalt des Buffers 
im Fenster Sichtbar wird. Auskommentieren von glBlitFramebuffer führt zu 
einem blauen Fenster.

[Daniel A. (daniel-a)]

Ich habe ein lauffähiges Minimalbeispiel erstellt, welches das selbe 
Verhalten zeigt. Es befindet sich im Anhang.

Systemanforderungen:
 * Linux
 * C-Compiler mit C99 Support
 * OpenGL >= 3.3
 * OpenCL >= 1.1