Changes between Version 8 and Version 9 of OpenCLTransformation

Timestamp:

07/11/14 09:47:19 (12 years ago)

Author:

fuufusuu

Comment:

--

OpenCLTransformation

@@ -9 +9 @@
 This only takes up the 3rd and 4th parameter, the 3rd for the number of devices, but also uses the name of the pointer in the 4th place. Note that the part for picking a device actually comes from clCreateCommandQueue, and if multiple devices are not used then the device at index 0 is used
 {{{
-int device_id[NUM_DEVICES];
-  //put device_ids
-  for(int i = 0; i < NUM_DEVICES; i++)
-  {
-    device_id[i] = i;
+int clGetDeviceIDs(int numEntries, cl_device_id * devices)
+{
+  for (int i=0; i<numEntries; i++) {
+    devices[i].id = i;
+    // exactly equivalent to: (devices+i)->id = i
   }
+  return CL_SUCCESS;
+}
 }}}
 
 kernel = clCreateKernel(program, "square", &err);
 
-Creates the kernel using data from the program, and the name of the function. In the transformation it chooses which function to use. Currently unimplemented.
+Creates the kernel using data from the program, and the name of the function. In the transformation it chooses which function to use. 
+
+{{{
+cl_kernel clCreateKernel(args * argument)
+{
+  cl_kernel kernel;
+  kernel.arguments = argument;
+  
+  return kernel;
+}
+}}}
+
+args is a struct containing all of the variables that will be passed into a kernel, for example
+{{{
+typedef struct
+{
+  //Variables for kernels
+  
+  float * input;
+  float * output;
+  int count;
+  
+}args;
+}}}
 
 input = clCreateBuffer(context,  CL_MEM_READ_ONLY,  sizeof(float) * count, NULL, NULL);
@@ -41 +66 @@
 clSetKernelArg sets arguments for an array of each device in the kernel. 
 {{{
-  $assert(global%local == 0);
-  kernel param[global/local];
-  for(int i = 0; i < global/local; i++)
-  {
-  //Also picks the device to be used
-    param[i].device_id = device_id[0];
-    //other parts of the struct
-    param[i].input = input;
-    param[i].output = output;
-    param[i].count = count;
-  }
+  ((args*)kernel.arguments)->input = input;
+  
+  ((args*)kernel.arguments)->output = output;
+
+  ((args*)kernel.arguments)->count = count;
 }}}
 
@@ -66 +85 @@
 
 {{{
+  int clEnqueueNDRangeKernel(cl_command_queue commands, cl_kernel kernel, int global, int local)
+{
+  $assert(global % local == 0);
+  cl_kernel param[global/local];
   $proc procs[global/local];
   for(int i = 0; i < global/local; i++)
   {
+    param[i] = kernel;
     param[i].workgroup = i;
-    //procs[i] = $spawn square(param[i].global_id, param[i].input, param[i].output, param[i].count);
-    procs[i] = $spawn worksquare(local, global, param[i]);
+    procs[i] = $spawn workfunc(local, global, param[i]);
   }
   
+  //this part here is the new clFinish(commands);
   for(int i = 0; i < global/local; i++)
   {
     $wait(procs[i]);
   }
+  
+  return CL_SUCCESS;
+}
 }}}