1 Reply Latest reply on Oct 4, 2012 6:44 AM by thejascr

    question about clSetEventCallBack

    thejascr

      Hi,

       

          I have a question regarding clSetEventCallBack() and the way callbacks work.

          I run the following code.

          =============================================================================

       

        int global_var = 0;

       

         void call_back(void * args)

         {

             global_var = 1;

          }

       

          begin_comp_copy_time = rtclock();

            clEnqueueNDRangeKernel(...,&compute_event);  // enqueue some computation

            clEnqueueReadBuffer(data_queue, CL_FALSE,....,1, &compute_event, &read_event);  // perform some read (non-blocking)

            clSetEventCallBack(read_event,..., call_back, args); // set a call back once the read finishes.

            clFinish(compute_queue);

            clFinish(data_queue);   // at this point all commands on all queues have completed.

          total_comp_copy_time = rtclock() - begin_comp_copy_time;

         

          begin_callback_time = rtclock();

              while(!global_var); // spin until the global_var is set to 1

          total_callback_time = rtclock() - begin_time;

         

          ==============================================================================

         

          When I print the timings, I see that total_comp_copy_time is just 3ms, but the total_callback_time is a whoophing 17ms.

         

          I am not able to reason out precisely the reason for this.(I am suspecting that this exceedingly high time is due to process scheduling issue)

          Can anyone precisely reason out the cause for this high timing values ?

          On what processor does the callback execute? is it the same processor as the one which registered the callback?

          If the processor is spinning in while loop, is the call_back waiting for the process to get scheduled out? is this the reason for 17ms?

       

          Thanks

          -Thejas

        • Re: question about clSetEventCallBack
          thejascr

          I have refined the code further to pin down to the smallest piece of code causing this

          problem. There is no need of running Kernel too.


          ======================================

          int global_var = 0;


          void call_back(void * args)

          {

          global_var = 1;

          }


          int main()

          {

          ....

          clEnqueueReadBuffer(data_queue, CL_FALSE,....,0, 0, &read_event); // perform some non-blocking read


          clSetEventCallBack(read_event,..., call_back, args); // set a call back once the read finishes.


          begin_callback_time = rtclock();

          while(!global_var); // spin until the global_var is set to 1

          total_callback_time = rtclock() - begin_time;


          }


          =================================================


          The above code is enough to hit a timing of 20ms. (though it only takes 2ms for actual data transfer). so only if I try to synchronize the callback (with "while") I am seeing this issue.

          If I dont try to synchronize, (I want to synchronize because I want to run this code in

          a loop and I dont want to go to the next iteration before this iteration's data is copied out)


          Any thoughts on what might be the reason?