ViewVC Help
View File | Revision Log | Show Annotations | Download File
/cvs/OpenCL/OpenCL.pm
(Generate patch)

Comparing OpenCL/OpenCL.pm (file contents):
Revision 1.38 by root, Thu Apr 19 19:36:24 2012 UTC vs.
Revision 1.47 by root, Sat Apr 21 19:48:58 2012 UTC

… …
160 '; 160 ';
161 161
162 my $prog = $ctx->program_with_source ($src); 162 my $prog = $ctx->program_with_source ($src);
163 163
164 # build croaks on compile errors, so catch it and print the compile errors 164 # build croaks on compile errors, so catch it and print the compile errors
165 eval { $prog->build ($dev); 1 } 165 eval { $prog->build ($dev, "-cl-fast-relaxed-math"); 1 }
166 or die $prog->build_log; 166 or die $prog->build_log;
167 167
168 my $kernel = $prog->kernel ("squareit"); 168 my $kernel = $prog->kernel ("squareit");
169 169
170=head2 Create some input and output float buffers, then call the 170=head2 Create some input and output float buffers, then call the
… …
260 m.x = fabs (fmod (m.x + time * 0.05f, 4.f)) - 2.f; 260 m.x = fabs (fmod (m.x + time * 0.05f, 4.f)) - 2.f;
261 261
262 float2 z = m; 262 float2 z = m;
263 float2 c = (float2)(sin (time * 0.05005), cos (time * 0.06001)); 263 float2 c = (float2)(sin (time * 0.05005), cos (time * 0.06001));
264 264
265 for (int i = 0; i < 100 && dot (z, z) < 4.f; ++i) 265 for (int i = 0; i < 25 && dot (z, z) < 4.f; ++i)
266 z = (float2)(z.x * z.x - z.y * z.y, 2.f * z.x * z.y) + c; 266 z = (float2)(z.x * z.x - z.y * z.y, 2.f * z.x * z.y) + c;
267 267
268 float3 colour = (float3)(z.x, z.y, z.x * z.y); 268 float3 colour = (float3)(z.x, z.y, z.x * z.y);
269 write_imagef (img, (int2)(get_global_id (0), get_global_id (1)), (float4)(colour * p.x * p.x, 1.)); 269 write_imagef (img, (int2)(get_global_id (0), get_global_id (1)), (float4)(colour * p.x * p.x, 1.));
270 } 270 }
… …
288 288
289 # release objects to opengl again 289 # release objects to opengl again
290 $queue->enqueue_release_gl_objects ([$tex]); 290 $queue->enqueue_release_gl_objects ([$tex]);
291 291
292 # wait 292 # wait
293 $queue->flush; 293 $queue->finish;
294 294
295 # now draw the texture, the defaults should be all right 295 # now draw the texture, the defaults should be all right
296 glTexParameterf GL_TEXTURE_2D, GL_TEXTURE_MIN_FILTER, GL_NEAREST; 296 glTexParameterf GL_TEXTURE_2D, GL_TEXTURE_MIN_FILTER, GL_NEAREST;
297 297
298 glEnable GL_TEXTURE_2D; 298 glEnable GL_TEXTURE_2D;
… …
336=item * Structures are often specified by flattening out their components 336=item * Structures are often specified by flattening out their components
337as with short vectors, and returned as arrayrefs. 337as with short vectors, and returned as arrayrefs.
338 338
339=item * When enqueuing commands, the wait list is specified by adding 339=item * When enqueuing commands, the wait list is specified by adding
340extra arguments to the function - anywhere a C<$wait_events...> argument 340extra arguments to the function - anywhere a C<$wait_events...> argument
341is documented this can be any number of event objects. 341is documented this can be any number of event objects. As an extsnion
342implemented by this module, C<undef> values will be ignored in the event
343list.
342 344
343=item * When enqueuing commands, if the enqueue method is called in void 345=item * When enqueuing commands, if the enqueue method is called in void
344context, no event is created. In all other contexts an event is returned 346context, no event is created. In all other contexts an event is returned
345by the method. 347by the method.
346 348
… …
748 750
749=item @device_partition_property_exts = $device->affinity_domains_ext 751=item @device_partition_property_exts = $device->affinity_domains_ext
750 752
751Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result. 753Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.
752 754
753=item $uint = $device->reference_count_ext 755=item $uint = $device->reference_count_ext
754 756
755Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT > and returns the result. 757Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT > and returns the result.
756 758
757=item @device_partition_property_exts = $device->partition_style_ext 759=item @device_partition_property_exts = $device->partition_style_ext
758 760
… …
769=item $queue = $ctx->queue ($device, $properties) 771=item $queue = $ctx->queue ($device, $properties)
770 772
771Create a new OpenCL::Queue object from the context and the given device. 773Create a new OpenCL::Queue object from the context and the given device.
772 774
773L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html> 775L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html>
776
777Example: create an out-of-order queue.
778
779 $queue = $ctx->queue ($device, OpenCL::QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE);
774 780
775=item $ev = $ctx->user_event 781=item $ev = $ctx->user_event
776 782
777Creates a new OpenCL::UserEvent object. 783Creates a new OpenCL::UserEvent object.
778 784
… …
809Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given 815Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given
810OpenGL buffer object. 816OpenGL buffer object.
811 817
812http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html 818http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html
813 819
820=item $img = $ctx->gl_texture ($flags, $target, $miplevel, $texture)
821
822Creates a new OpenCL::Image object that refers to the given OpenGL
823texture object or buffer.
824
825http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateFromGLTexture.html
826
814=item $ctx->gl_texture2d ($flags, $target, $miplevel, $texture) 827=item $img = $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)
815 828
816Creates a new OpenCL::Image2D object that refers to the given OpenGL 829Creates a new OpenCL::Image2D object that refers to the given OpenGL
8172D texture object. 8302D texture object.
818 831
819http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture2D.html 832http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture2D.html
820 833
821=item $ctx->gl_texture3d ($flags, $target, $miplevel, $texture) 834=item $img = $ctx->gl_texture3d ($flags, $target, $miplevel, $texture)
822 835
823Creates a new OpenCL::Image3D object that refers to the given OpenGL 836Creates a new OpenCL::Image3D object that refers to the given OpenGL
8243D texture object. 8373D texture object.
825 838
826http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture3D.html 839http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture3D.html
… …
889for completion, unless the method is called in void context, in which case 902for completion, unless the method is called in void context, in which case
890no event object is created. 903no event object is created.
891 904
892They also allow you to specify any number of other event objects that this 905They also allow you to specify any number of other event objects that this
893request has to wait for before it starts executing, by simply passing the 906request has to wait for before it starts executing, by simply passing the
894event objects as extra parameters to the enqueue methods. 907event objects as extra parameters to the enqueue methods. To simplify
908program design, this module ignores any C<undef> values in the list of
909events. This makes it possible to code operations such as this, without
910having to put a valid event object into C<$event> first:
911
912 $event = $queue->enqueue_xxx (..., $event);
895 913
896Queues execute in-order by default, without any parallelism, so in most 914Queues execute in-order by default, without any parallelism, so in most
897cases (i.e. you use only one queue) it's not necessary to wait for or 915cases (i.e. you use only one queue) it's not necessary to wait for or
898create event objects. 916create event objects, althoguh an our of order queue is often a bit
917faster.
899 918
900=over 4 919=over 4
901 920
902=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...) 921=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...)
903 922
… …
969reference to an array of local work sizes, with the same number of 988reference to an array of local work sizes, with the same number of
970elements as @$global_work_size. 989elements as @$global_work_size.
971 990
972L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html> 991L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>
973 992
974=item $ev = $queue->enqueue_marker ($wait_events...)
975
976L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMarker.html>
977
978=item $ev = $queue->enqueue_acquire_gl_objects ([object, ...], $wait_events...) 993=item $ev = $queue->enqueue_acquire_gl_objects ([object, ...], $wait_events...)
979 994
980Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired 995Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired
981for subsequent OpenCL usage. 996for subsequent OpenCL usage.
982 997
… …
991 1006
992=item $ev = $queue->enqueue_wait_for_events ($wait_events...) 1007=item $ev = $queue->enqueue_wait_for_events ($wait_events...)
993 1008
994L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWaitForEvents.html> 1009L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWaitForEvents.html>
995 1010
996=item $queue->enqueue_barrier 1011=item $ev = $queue->enqueue_marker ($wait_events...)
997 1012
1013L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueMarkerWithWaitList.html>
1014
1015=item $ev = $queue->enqueue_barrier ($wait_events...)
1016
998L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueBarrier.html> 1017L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueBarrierWithWaitList.html>
999 1018
1000=item $queue->flush 1019=item $queue->flush
1001 1020
1002L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFlush.html> 1021L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFlush.html>
1003 1022
… …
1118 1137
1119=back 1138=back
1120 1139
1121=head2 THE OpenCL::Image CLASS 1140=head2 THE OpenCL::Image CLASS
1122 1141
1123This is the superclass of all image objects - OpenCL::Image2D and OpenCL::Image3D. 1142This is the superclass of all image objects - OpenCL::Image1D,
1143OpenCL::Image1DArray, OpenCL::Image1DBuffer, OpenCL::Image2D,
1144OpenCL::Image2DArray and OpenCL::Image3D.
1124 1145
1125=over 4 1146=over 4
1126 1147
1127=item $packed_value = $ev->image_info ($name) 1148=item $packed_value = $ev->image_info ($name)
1128 1149
… …
1369 1390
1370This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>. 1391This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>.
1371 1392
1372TYPE is one of C<char>, C<uchar>, C<short>, C<ushort>, C<int>, C<uint>, 1393TYPE is one of C<char>, C<uchar>, C<short>, C<ushort>, C<int>, C<uint>,
1373C<long>, C<ulong>, C<half>, C<float>, C<double>, C<memory>, C<buffer>, 1394C<long>, C<ulong>, C<half>, C<float>, C<double>, C<memory>, C<buffer>,
1374C<image2d>, C<image3d>, C<sampler> or C<event>. 1395C<image2d>, C<image3d>, C<sampler>, C<local> or C<event>.
1375 1396
1376Chars and integers (including the half type) are specified as integers, 1397Chars and integers (including the half type) are specified as integers,
1377float and double as floating point values, memory/buffer/image2d/image3d 1398float and double as floating point values, memory/buffer/image2d/image3d
1378must be an object of that type or C<undef>, and sampler and event must be 1399must be an object of that type or C<undef>, local-memory arguments are
1379objects of that type. 1400set by specifying the size, and sampler and event must be objects of that
1401type.
1380 1402
1381L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetKernelArg.html> 1403L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetKernelArg.html>
1382 1404
1383=back 1405=back
1384 1406
… …
1473package OpenCL; 1495package OpenCL;
1474 1496
1475use common::sense; 1497use common::sense;
1476 1498
1477BEGIN { 1499BEGIN {
1478 our $VERSION = '0.95'; 1500 our $VERSION = '0.96';
1479 1501
1480 require XSLoader; 1502 require XSLoader;
1481 XSLoader::load (__PACKAGE__, $VERSION); 1503 XSLoader::load (__PACKAGE__, $VERSION);
1482 1504
1483 @OpenCL::Buffer::ISA = 1505 @OpenCL::Buffer::ISA =
1484 @OpenCL::Image::ISA = OpenCL::Memory::; 1506 @OpenCL::Image::ISA = OpenCL::Memory::;
1485 1507
1486 @OpenCL::BufferObj::ISA = OpenCL::Buffer::; 1508 @OpenCL::BufferObj::ISA = OpenCL::Buffer::;
1487 1509
1488 @OpenCL::Image2D::ISA = 1510 @OpenCL::Image2D::ISA =
1511 @OpenCL::Image3D::ISA =
1512 @OpenCL::Image2DArray::ISA =
1513 @OpenCL::Image1D::ISA =
1514 @OpenCL::Image1DArray::ISA =
1489 @OpenCL::Image3D::ISA = OpenCL::Image::; 1515 @OpenCL::Image1DBuffer::ISA = OpenCL::Image::;
1490 1516
1491 @OpenCL::UserEvent::ISA = OpenCL::Event::; 1517 @OpenCL::UserEvent::ISA = OpenCL::Event::;
1492} 1518}
1493 1519
14941; 15201;
1495 1521
1496=head1 AUTHOR 1522=head1 AUTHOR

Diff Legend

– Removed lines
+ Added lines
< Changed lines
> Changed lines