ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/OpenCL/OpenCL.pm

Comparing OpenCL/OpenCL.pm (file contents):
Revision 1.20 by root, Sun Nov 20 01:09:48 2011 UTC vs.
Revision 1.56 by root, Tue Apr 24 23:53:12 2012 UTC

…		…
101		101
102	Best run this once to get a feel for the platforms and devices in your	102	Best run this once to get a feel for the platforms and devices in your
103	system.	103	system.
104		104
105	for my $platform (OpenCL::platforms) {	105	for my $platform (OpenCL::platforms) {
106	printf "platform: %s\n", $platform->info (OpenCL::PLATFORM_NAME);	106	printf "platform: %s\n", $platform->name;
107	printf "extensions: %s\n", $platform->info (OpenCL::PLATFORM_EXTENSIONS);	107	printf "extensions: %s\n", $platform->extensions;
108	for my $device ($platform->devices) {	108	for my $device ($platform->devices) {
109	printf "+ device: %s\n", $device->info (OpenCL::DEVICE_NAME);	109	printf "+ device: %s\n", $device->name;
110	my $ctx = $device->context;	110	my $ctx = $platform->context (undef, [$device]);
111	# do stuff	111	# do stuff
112	}	112	}
113	}	113	}
114		114
115	=head2 Get a useful context and a command queue.	115	=head2 Get a useful context and a command queue.
…		…
149		149
150	=head2 Create and build a program, then create a kernel out of one of its	150	=head2 Create and build a program, then create a kernel out of one of its
151	functions.	151	functions.
152		152
153	my $src = '	153	my $src = '
154	__kernel void	154	kernel void
155	squareit (__global float *input, __global float *output)	155	squareit (global float *input, global float *output)
156	{	156	{
157	$id = get_global_id (0);	157	$id = get_global_id (0);
158	output [id] = input [id] * input [id];	158	output [id] = input [id] * input [id];
159	}	159	}
160	';	160	';
161		161
162	my $prog = $ctx->program_with_source ($src);	162	my $prog = $ctx->build_program ($src);
163
164	# build croaks on compile errors, so catch it and print the compile errors
165	eval { $prog->build ($dev); 1 }
166	or die $prog->build_info ($dev, OpenCL::PROGRAM_BUILD_LOG);
167
168	my $kernel = $prog->kernel ("squareit");	163	my $kernel = $prog->kernel ("squareit");
169		164
170	=head2 Create some input and output float buffers, then call the	165	=head2 Create some input and output float buffers, then call the
171	'squareit' kernel on them.	166	'squareit' kernel on them.
172		167
…		…
210	# enqueue an async read	205	# enqueue an async read
211	$ev = $queue->enqueue_read_buffer ($output, 0, 0, OpenCL::SIZEOF_FLOAT * 4, my $data, $ev);	206	$ev = $queue->enqueue_read_buffer ($output, 0, 0, OpenCL::SIZEOF_FLOAT * 4, my $data, $ev);
212		207
213	# wait for the last event to complete	208	# wait for the last event to complete
214	$ev->wait;	209	$ev->wait;
		210
		211	=head2 Use the OpenGL module to share a texture between OpenCL and OpenGL and draw some julia
		212	set tunnel effect.
		213
		214	This is quite a long example to get you going.
		215
		216	use OpenGL ":all";
		217	use OpenCL;
		218
		219	# open a window and create a gl texture
		220	OpenGL::glpOpenWindow width => 256, height => 256;
		221	my $texid = glGenTextures_p 1;
		222	glBindTexture GL_TEXTURE_2D, $texid;
		223	glTexImage2D_c GL_TEXTURE_2D, 0, GL_RGBA8, 256, 256, 0, GL_RGBA, GL_UNSIGNED_BYTE, 0;
		224
		225	# find and use the first opencl device that let's us get a shared opengl context
		226	my $platform;
		227	my $dev;
		228	my $ctx;
		229
		230	for (OpenCL::platforms) {
		231	$platform = $_;
		232	for ($platform->devices) {
		233	$dev = $_;
		234	$ctx = $platform->context ([OpenCL::GLX_DISPLAY_KHR, undef, OpenCL::GL_CONTEXT_KHR, undef], [$dev])
		235	and last;
		236	}
		237	}
		238
		239	$ctx
		240	or die "cannot find suitable OpenCL device\n";
		241
		242	my $queue = $ctx->queue ($dev);
		243
		244	# now attach an opencl image2d object to the opengl texture
		245	my $tex = $ctx->gl_texture2d (OpenCL::MEM_WRITE_ONLY, GL_TEXTURE_2D, 0, $texid);
		246
		247	# now the boring opencl code
		248	my $src = <<EOF;
		249	kernel void
		250	juliatunnel (write_only image2d_t img, float time)
		251	{
		252	float2 p = (float2)(get_global_id (0), get_global_id (1)) / 256.f * 2.f - 1.f;
		253
		254	float2 m = (float2)(1.f, p.y) / fabs (p.x);
		255	m.x = fabs (fmod (m.x + time * 0.05f, 4.f)) - 2.f;
		256
		257	float2 z = m;
		258	float2 c = (float2)(sin (time * 0.05005), cos (time * 0.06001));
		259
		260	for (int i = 0; i < 25 && dot (z, z) < 4.f; ++i)
		261	z = (float2)(z.x * z.x - z.y * z.y, 2.f * z.x * z.y) + c;
		262
		263	float3 colour = (float3)(z.x, z.y, z.x * z.y);
		264	write_imagef (img, (int2)(get_global_id (0), get_global_id (1)), (float4)(colour * p.x * p.x, 1.));
		265	}
		266	EOF
		267
		268	my $prog = $ctx->build_program ($src);
		269	my $kernel = $prog->kernel ("juliatunnel");
		270
		271	# program compiled, kernel ready, now draw and loop
		272
		273	for (my $time; ; ++$time) {
		274	# acquire objects from opengl
		275	$queue->enqueue_acquire_gl_objects ([$tex]);
		276
		277	# configure and run our kernel
		278	$kernel->set_image2d (0, $tex);
		279	$kernel->set_float (1, $time);
		280	$queue->enqueue_nd_range_kernel ($kernel, undef, [256, 256], undef);
		281
		282	# release objects to opengl again
		283	$queue->enqueue_release_gl_objects ([$tex]);
		284
		285	# wait
		286	$queue->finish;
		287
		288	# now draw the texture, the defaults should be all right
		289	glTexParameterf GL_TEXTURE_2D, GL_TEXTURE_MIN_FILTER, GL_NEAREST;
		290
		291	glEnable GL_TEXTURE_2D;
		292	glBegin GL_QUADS;
		293	glTexCoord2f 0, 1; glVertex3i -1, -1, -1;
		294	glTexCoord2f 0, 0; glVertex3i 1, -1, -1;
		295	glTexCoord2f 1, 0; glVertex3i 1, 1, -1;
		296	glTexCoord2f 1, 1; glVertex3i -1, 1, -1;
		297	glEnd;
		298
		299	glXSwapBuffers;
		300
		301	select undef, undef, undef, 1/60;
		302	}
215		303
216	=head1 DOCUMENTATION	304	=head1 DOCUMENTATION
217		305
218	=head2 BASIC CONVENTIONS	306	=head2 BASIC CONVENTIONS
219		307
…		…
241	=item * Structures are often specified by flattening out their components	329	=item * Structures are often specified by flattening out their components
242	as with short vectors, and returned as arrayrefs.	330	as with short vectors, and returned as arrayrefs.
243		331
244	=item * When enqueuing commands, the wait list is specified by adding	332	=item * When enqueuing commands, the wait list is specified by adding
245	extra arguments to the function - anywhere a C<$wait_events...> argument	333	extra arguments to the function - anywhere a C<$wait_events...> argument
246	is documented this can be any number of event objects.	334	is documented this can be any number of event objects. As an extsnion
		335	implemented by this module, C<undef> values will be ignored in the event
		336	list.
247		337
248	=item * When enqueuing commands, if the enqueue method is called in void	338	=item * When enqueuing commands, if the enqueue method is called in void
249	context, no event is created. In all other contexts an event is returned	339	context, no event is created. In all other contexts an event is returned
250	by the method.	340	by the method.
251		341
…		…
271	ulong IV - Q	361	ulong IV - Q
272	float NV float f	362	float NV float f
273	half IV ushort S	363	half IV ushort S
274	double NV double d	364	double NV double d
275		365
		366	=head2 GLX SUPPORT
		367
		368	Due to the sad state that OpenGL support is in in Perl (mostly the OpenGL
		369	module, which has little to no documentation and has little to no support
		370	for glX), this module, as a special extension, treats context creation
		371	properties C<OpenCL::GLX_DISPLAY_KHR> and C<OpenCL::GL_CONTEXT_KHR>
		372	specially: If either or both of these are C<undef>, then the OpenCL
		373	module tries to dynamically resolve C<glXGetCurrentDisplay> and
		374	C<glXGetCurrentContext>, call these functions and use their return values
		375	instead.
		376
		377	For this to work, the OpenGL library must be loaded, a GLX context must
		378	have been created and be made current, and C<dlsym> must be available and
		379	capable of finding the function via C<RTLD_DEFAULT>.
		380
		381	=head2 EVENT SYSTEM
		382
		383	OpenCL can generate a number of (potentially) asynchronous events, for
		384	example, after compiling a program, to signal a context-related error or,
		385	perhaps most important, to signal completion of queued jobs (by setting
		386	callbacks on OpenCL::Event objects).
		387
		388	To facilitate this, this module maintains an event queue - each
		389	time an asynchronous event happens, it is queued, and perl will be
		390	interrupted. This is implemented via the L<Async::Interrupt> module. In
		391	addition, this module has L<AnyEvent> support, so it can seamlessly
		392	integrate itself into many event loops.
		393
		394	Since this module is a bit hard to understand, here are some case examples:
		395
		396	=head3 Don't use callbacks.
		397
		398	When your program never uses any callbacks, then there will never be any
		399	notifications you need to take care of, and therefore no need to worry
		400	about all this.
		401
		402	You can achieve a great deal by explicitly waiting for events, or using
		403	barriers and flush calls. In many programs, there is no need at all to
		404	tinker with asynchronous events.
		405
		406	=head3 Use AnyEvent
		407
		408	This module automatically registers a watcher that invokes all outstanding
		409	event callbacks when AnyEvent is initialised (and block asynchronous
		410	interruptions). Using this mode of operations is the safest and most
		411	recommended one.
		412
		413	To use this, simply use AnyEvent and this module normally, make sure you
		414	have an event loop running:
		415
		416	use Gtk2 -init;
		417	use AnyEvent;
		418
		419	# initialise AnyEvent, by creating a watcher, or:
		420	AnyEvent::detect;
		421
		422	my $e = $queue->enqueue_marker;
		423	$e->cb (sub {
		424	warn "opencl is finished\n";
		425	})
		426
		427	main Gtk2;
		428
		429	Note that this module will not initialise AnyEvent for you. Before
		430	AnyEvent is initialised, the module will asynchronously interrupt perl
		431	instead. To avoid any surprises, it's best to explicitly initialise
		432	AnyEvent.
		433
		434	You can temporarily enable asynchronous interruptions (see next paragraph)
		435	by calling C<$OpenCL::INTERRUPT->unblock> and disable them again by
		436	calling C<$OpenCL::INTERRUPT->block>.
		437
		438	=head3 Let yourself be interrupted at any time
		439
		440	This mode is the default unless AnyEvent is loaded and initialised. In
		441	this mode, OpenCL asynchronously interrupts a running perl program. The
		442	emphasis is on both I<asynchronously> and I<running> here.
		443
		444	Asynchronously means that perl might execute your callbacks at any
		445	time. For example, in the following code (I<THAT YOU SHOULD NOT COPY>),
		446	the C<until> loop following the marker call will be interrupted by the
		447	callback:
		448
		449	my $e = $queue->enqueue_marker;
		450	my $flag;
		451	$e->cb (sub { $flag = 1 });
		452	1 until $flag;
		453	# $flag is now 1
		454
		455	The reason why you shouldn't blindly copy the above code is that
		456	busy waiting is a really really bad thing, and really really bad for
		457	performance.
		458
		459	While at first this asynchronous business might look exciting, it can be
		460	really hard, because you need to be prepared for the callback code to be
		461	executed at any time, which limits the amount of things the callback code
		462	can do safely.
		463
		464	This can be mitigated somewhat by using C<<
		465	$OpenCL::INTERRUPT->scope_block >> (see the L<Async::Interrupt>
		466	documentation for details).
		467
		468	The other problem is that your program must be actively I<running> to be
		469	interrupted. When you calculate stuff, your program is running. When you
		470	hang in some C functions or other block execution (by calling C<sleep>,
		471	C<select>, running an event loop and so on), your program is waiting, not
		472	running.
		473
		474	One way around that would be to attach a read watcher to your event loop,
		475	listening for events on C<< $OpenCL::INTERRUPT->pipe_fileno >>, using a
		476	dummy callback (C<sub { }>) to temporarily execute some perl code.
		477
		478	That is then awfully close to using the built-in AnyEvent support above,
		479	though, so consider that one instead.
		480
		481	=head3 Be creative
		482
		483	OpenCL exports the L<Async::Interrupt> object it uses in the global
		484	variable C<$OpenCL::INTERRUPT>. You can configure it in any way you like.
		485
		486	So if you want to feel like a real pro, err, wait, if you feel no risk
		487	menas no fun, you can experiment by implementing your own mode of
		488	operations.
		489
		490	=cut
		491
		492	package OpenCL;
		493
		494	use common::sense;
		495	use Async::Interrupt ();
		496
		497	our $POLL_FUNC; # set by XS
		498
		499	BEGIN {
		500	our $VERSION = '0.97';
		501
		502	require XSLoader;
		503	XSLoader::load (__PACKAGE__, $VERSION);
		504
		505	@OpenCL::Platform::ISA =
		506	@OpenCL::Device::ISA =
		507	@OpenCL::Context::ISA =
		508	@OpenCL::Queue::ISA =
		509	@OpenCL::Memory::ISA =
		510	@OpenCL::Sampler::ISA =
		511	@OpenCL::Program::ISA =
		512	@OpenCL::Kernel::ISA =
		513	@OpenCL::Event::ISA = OpenCL::Object::;
		514
		515	@OpenCL::Buffer::ISA =
		516	@OpenCL::Image::ISA = OpenCL::Memory::;
		517
		518	@OpenCL::BufferObj::ISA = OpenCL::Buffer::;
		519
		520	@OpenCL::Image2D::ISA =
		521	@OpenCL::Image3D::ISA =
		522	@OpenCL::Image2DArray::ISA =
		523	@OpenCL::Image1D::ISA =
		524	@OpenCL::Image1DArray::ISA =
		525	@OpenCL::Image1DBuffer::ISA = OpenCL::Image::;
		526
		527	@OpenCL::UserEvent::ISA = OpenCL::Event::;
		528	}
		529
276	=head2 THE OpenCL PACKAGE	530	=head2 THE OpenCL PACKAGE
277		531
278	=over 4	532	=over 4
279		533
280	=item $int = OpenCL::errno	534	=item $int = OpenCL::errno
…		…
286		540
287	Comverts an error value into a human readable string.	541	Comverts an error value into a human readable string.
288		542
289	=item $str = OpenCL::enum2str $enum	543	=item $str = OpenCL::enum2str $enum
290		544
291	Converts most enum values (inof parameter names, image format constants,	545	Converts most enum values (of parameter names, image format constants,
292	object types, addressing and filter modes, command types etc.) into a	546	object types, addressing and filter modes, command types etc.) into a
293	human readbale string. When confronted with some random integer it can be	547	human readable string. When confronted with some random integer it can be
294	very helpful to pass it through this function to maybe get some readable	548	very helpful to pass it through this function to maybe get some readable
295	string out of it.	549	string out of it.
296		550
297	=item @platforms = OpenCL::platforms	551	=item @platforms = OpenCL::platforms
298		552
299	Returns all available OpenCL::Platform objects.	553	Returns all available OpenCL::Platform objects.
300		554
301	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformIDs.html>	555	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformIDs.html>
302		556
303	=item $ctx = OpenCL::context_from_type $properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $notify = undef	557	=item $ctx = OpenCL::context_from_type $properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $callback->($err, $pvt) = $print_stderr
304		558
305	Tries to create a context from a default device and platform - never worked for me.	559	Tries to create a context from a default device and platform type - never worked for me.
306		560
307	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>	561	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>
308		562
		563	=item $ctx = OpenCL::context $properties, \@devices, $callback->($err, $pvt) = $print_stderr)
		564
		565	Create a new OpenCL::Context object using the given device object(s). This
		566	function isn't implemented yet, use C<< $platform->context >> instead.
		567
		568	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>
		569
309	=item OpenCL::wait_for_events $wait_events...	570	=item OpenCL::wait_for_events $wait_events...
310		571
311	Waits for all events to complete.	572	Waits for all events to complete.
312		573
313	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clWaitForEvents.html>	574	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clWaitForEvents.html>
314		575
		576	=item OpenCL::poll
		577
		578	Checks if there are any outstanding events (see L<EVENT SYSTEM>) and
		579	invokes their callbacks.
		580
		581	=item $OpenCL::INTERRUPT
		582
		583	The L<Async::Interrupt> object used to signal asynchronous events (see
		584	L<EVENT SYSTEM>).
		585
		586	=cut
		587
		588	our $INTERRUPT = new Async::Interrupt c_cb => [$POLL_FUNC, 0];
		589
		590	&_eq_initialise ($INTERRUPT->signal_func);
		591
		592	=item $OpenCL::WATCHER
		593
		594	The L<AnyEvent> watcher object used to watch for asynchronous events (see
		595	L<EVENT SYSTEM>). This variable is C<undef> until L<AnyEvent> has been
		596	loaded I<and> initialised (e.g. by calling C<AnyEvent::detect>).
		597
		598	=cut
		599
		600	our $WATCHER;
		601
		602	sub _init_anyevent {
		603	$INTERRUPT->block;
		604	$WATCHER = AE::io ($INTERRUPT->pipe_fileno, 0, sub { $INTERRUPT->handle });
		605	}
		606
		607	if (defined $AnyEvent::MODEL) {
		608	_init_anyevent;
		609	} else {
		610	push @AnyEvent::post_detect, \&_init_anyevent;
		611	}
		612
315	=back	613	=back
316		614
		615	=head2 THE OpenCL::Object CLASS
		616
		617	This is the base class for all objects in the OpenCL module. The only
		618	method it implements is the C<id> method, which is only useful if you want
		619	to interface to OpenCL on the C level.
		620
		621	=over 4
		622
		623	=item $iv = $obj->id
		624
		625	OpenCL objects are represented by pointers or integers on the C level. If
		626	you want to interface to an OpenCL object directly on the C level, then
		627	you need this value, which is returned by this method. You should use an
		628	C<IV> type in your code and cast that to the correct type.
		629
		630	=cut
		631
		632	sub OpenCL::Object::id {
		633	ref $_[0] eq "SCALAR"
		634	? ${ $_[0] }
		635	: $_[0][0]
		636	}
		637
		638	=back
		639
317	=head2 THE OpenCL::Platform CLASS	640	=head2 THE OpenCL::Platform CLASS
318		641
319	=over 4	642	=over 4
320		643
321	=item @devices = $platform->devices ($type = OpenCL::DEVICE_TYPE_ALL)	644	=item @devices = $platform->devices ($type = OpenCL::DEVICE_TYPE_ALL)
322		645
323	Returns a list of matching OpenCL::Device objects.	646	Returns a list of matching OpenCL::Device objects.
324		647
325	=item $ctx = $platform->context_from_type ($properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $notify = undef)	648	=item $ctx = $platform->context_from_type ($properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $callback->($err, $pvt) = $print_stderr)
326		649
327	Tries to create a context. Never worked for me, and you need devices explitly anyway.	650	Tries to create a context. Never worked for me, and you need devices explicitly anyway.
328		651
329	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>	652	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>
330		653
331	=item $ctx = $device->context ($properties = undef, @$devices, $notify = undef)	654	=item $ctx = $platform->context ($properties, \@devices, $callback->($err, $pvt) = $print_stderr)
332		655
333	Create a new OpenCL::Context object using the given device object(s)- a	656	Create a new OpenCL::Context object using the given device object(s)- a
334	CL_CONTEXT_PLATFORM property is supplied automatically.	657	CL_CONTEXT_PLATFORM property is supplied automatically.
335		658
336	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>	659	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>
337		660
338	=item $packed_value = $platform->info ($name)	661	=item $packed_value = $platform->info ($name)
339		662
340	Calls C<clGetPlatformInfo> and returns the packed, raw value - for	663	Calls C<clGetPlatformInfo> and returns the packed, raw value - for
341	strings, this will be the string, for other values you probably need to	664	strings, this will be the string (possibly including terminating \0), for
342	use the correct C<unpack>.	665	other values you probably need to use the correct C<unpack>.
343		666
344	It's best to avoid this method and use one of the predefined C<get_*>	667	It's best to avoid this method and use one of the following convenience
345	methods.	668	wrappers.
346		669
347	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformInfo.html>	670	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformInfo.html>
348		671
		672	=item $platform->unload_compiler
		673
		674	Attempts to unload the compiler for this platform, for endless
		675	profit. Does nothing on OpenCL 1.1.
		676
		677	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clUnloadPlatformCompiler.html>
		678
349	=for gengetinfo begin platform	679	=for gengetinfo begin platform
350		680
351
352	=item $string = $platform->profile	681	=item $string = $platform->profile
353		682
354	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result(s).	683	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result.
355		684
356	=item $string = $platform->version	685	=item $string = $platform->version
357		686
358	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VERSION> and returns the result(s).	687	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VERSION> and returns the result.
359		688
360	=item $string = $platform->name	689	=item $string = $platform->name
361		690
362	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_NAME> and returns the result(s).	691	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_NAME> and returns the result.
363		692
364	=item $string = $platform->vendor	693	=item $string = $platform->vendor
365		694
366	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VENDOR> and returns the result(s).	695	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VENDOR> and returns the result.
367		696
368	=item $string = $platform->extensions	697	=item $string = $platform->extensions
369		698
370	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_EXTENSIONS> and returns the result(s).	699	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_EXTENSIONS> and returns the result.
		700
371	=for gengetinfo end platform	701	=for gengetinfo end platform
372		702
373	=back	703	=back
374		704
375	=head2 THE OpenCL::Device CLASS	705	=head2 THE OpenCL::Device CLASS
…		…
380		710
381	See C<< $platform->info >> for details.	711	See C<< $platform->info >> for details.
382		712
383	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetDeviceInfo.html>	713	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetDeviceInfo.html>
384		714
		715	=for gengetinfo begin device
		716
		717	=item $device_type = $device->type
		718
		719	Calls C<clGetDeviceInfo> with C<CL_DEVICE_TYPE> and returns the result.
		720
		721	=item $uint = $device->vendor_id
		722
		723	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR_ID> and returns the result.
		724
		725	=item $uint = $device->max_compute_units
		726
		727	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_COMPUTE_UNITS> and returns the result.
		728
		729	=item $uint = $device->max_work_item_dimensions
		730
		731	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS> and returns the result.
		732
		733	=item $int = $device->max_work_group_size
		734
		735	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_GROUP_SIZE> and returns the result.
		736
		737	=item @ints = $device->max_work_item_sizes
		738
		739	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_SIZES> and returns the result.
		740
		741	=item $uint = $device->preferred_vector_width_char
		742
		743	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR> and returns the result.
		744
		745	=item $uint = $device->preferred_vector_width_short
		746
		747	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT> and returns the result.
		748
		749	=item $uint = $device->preferred_vector_width_int
		750
		751	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT> and returns the result.
		752
		753	=item $uint = $device->preferred_vector_width_long
		754
		755	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG> and returns the result.
		756
		757	=item $uint = $device->preferred_vector_width_float
		758
		759	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT> and returns the result.
		760
		761	=item $uint = $device->preferred_vector_width_double
		762
		763	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE> and returns the result.
		764
		765	=item $uint = $device->max_clock_frequency
		766
		767	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CLOCK_FREQUENCY> and returns the result.
		768
		769	=item $bitfield = $device->address_bits
		770
		771	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ADDRESS_BITS> and returns the result.
		772
		773	=item $uint = $device->max_read_image_args
		774
		775	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_READ_IMAGE_ARGS> and returns the result.
		776
		777	=item $uint = $device->max_write_image_args
		778
		779	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WRITE_IMAGE_ARGS> and returns the result.
		780
		781	=item $ulong = $device->max_mem_alloc_size
		782
		783	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_MEM_ALLOC_SIZE> and returns the result.
		784
		785	=item $int = $device->image2d_max_width
		786
		787	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_WIDTH> and returns the result.
		788
		789	=item $int = $device->image2d_max_height
		790
		791	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_HEIGHT> and returns the result.
		792
		793	=item $int = $device->image3d_max_width
		794
		795	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_WIDTH> and returns the result.
		796
		797	=item $int = $device->image3d_max_height
		798
		799	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_HEIGHT> and returns the result.
		800
		801	=item $int = $device->image3d_max_depth
		802
		803	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_DEPTH> and returns the result.
		804
		805	=item $uint = $device->image_support
		806
		807	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE_SUPPORT> and returns the result.
		808
		809	=item $int = $device->max_parameter_size
		810
		811	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_PARAMETER_SIZE> and returns the result.
		812
		813	=item $uint = $device->max_samplers
		814
		815	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_SAMPLERS> and returns the result.
		816
		817	=item $uint = $device->mem_base_addr_align
		818
		819	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MEM_BASE_ADDR_ALIGN> and returns the result.
		820
		821	=item $uint = $device->min_data_type_align_size
		822
		823	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE> and returns the result.
		824
		825	=item $device_fp_config = $device->single_fp_config
		826
		827	Calls C<clGetDeviceInfo> with C<CL_DEVICE_SINGLE_FP_CONFIG> and returns the result.
		828
		829	=item $device_mem_cache_type = $device->global_mem_cache_type
		830
		831	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_TYPE> and returns the result.
		832
		833	=item $uint = $device->global_mem_cacheline_size
		834
		835	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE> and returns the result.
		836
		837	=item $ulong = $device->global_mem_cache_size
		838
		839	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_SIZE> and returns the result.
		840
		841	=item $ulong = $device->global_mem_size
		842
		843	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_SIZE> and returns the result.
		844
		845	=item $ulong = $device->max_constant_buffer_size
		846
		847	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE> and returns the result.
		848
		849	=item $uint = $device->max_constant_args
		850
		851	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_ARGS> and returns the result.
		852
		853	=item $device_local_mem_type = $device->local_mem_type
		854
		855	Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_TYPE> and returns the result.
		856
		857	=item $ulong = $device->local_mem_size
		858
		859	Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_SIZE> and returns the result.
		860
		861	=item $boolean = $device->error_correction_support
		862
		863	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ERROR_CORRECTION_SUPPORT> and returns the result.
		864
		865	=item $int = $device->profiling_timer_resolution
		866
		867	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILING_TIMER_RESOLUTION> and returns the result.
		868
		869	=item $boolean = $device->endian_little
		870
		871	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ENDIAN_LITTLE> and returns the result.
		872
		873	=item $boolean = $device->available
		874
		875	Calls C<clGetDeviceInfo> with C<CL_DEVICE_AVAILABLE> and returns the result.
		876
		877	=item $boolean = $device->compiler_available
		878
		879	Calls C<clGetDeviceInfo> with C<CL_DEVICE_COMPILER_AVAILABLE> and returns the result.
		880
		881	=item $device_exec_capabilities = $device->execution_capabilities
		882
		883	Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXECUTION_CAPABILITIES> and returns the result.
		884
		885	=item $command_queue_properties = $device->properties
		886
		887	Calls C<clGetDeviceInfo> with C<CL_DEVICE_QUEUE_PROPERTIES> and returns the result.
		888
		889	=item $ = $device->platform
		890
		891	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PLATFORM> and returns the result.
		892
		893	=item $string = $device->name
		894
		895	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NAME> and returns the result.
		896
		897	=item $string = $device->vendor
		898
		899	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR> and returns the result.
		900
		901	=item $string = $device->driver_version
		902
		903	Calls C<clGetDeviceInfo> with C<CL_DRIVER_VERSION> and returns the result.
		904
		905	=item $string = $device->profile
		906
		907	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILE> and returns the result.
		908
		909	=item $string = $device->version
		910
		911	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VERSION> and returns the result.
		912
		913	=item $string = $device->extensions
		914
		915	Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXTENSIONS> and returns the result.
		916
		917	=item $uint = $device->preferred_vector_width_half
		918
		919	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF> and returns the result.
		920
		921	=item $uint = $device->native_vector_width_char
		922
		923	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR> and returns the result.
		924
		925	=item $uint = $device->native_vector_width_short
		926
		927	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT> and returns the result.
		928
		929	=item $uint = $device->native_vector_width_int
		930
		931	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_INT> and returns the result.
		932
		933	=item $uint = $device->native_vector_width_long
		934
		935	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG> and returns the result.
		936
		937	=item $uint = $device->native_vector_width_float
		938
		939	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT> and returns the result.
		940
		941	=item $uint = $device->native_vector_width_double
		942
		943	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE> and returns the result.
		944
		945	=item $uint = $device->native_vector_width_half
		946
		947	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF> and returns the result.
		948
		949	=item $device_fp_config = $device->double_fp_config
		950
		951	Calls C<clGetDeviceInfo> with C<CL_DEVICE_DOUBLE_FP_CONFIG> and returns the result.
		952
		953	=item $device_fp_config = $device->half_fp_config
		954
		955	Calls C<clGetDeviceInfo> with C<CL_DEVICE_HALF_FP_CONFIG> and returns the result.
		956
		957	=item $boolean = $device->host_unified_memory
		958
		959	Calls C<clGetDeviceInfo> with C<CL_DEVICE_HOST_UNIFIED_MEMORY> and returns the result.
		960
		961	=item $device = $device->parent_device_ext
		962
		963	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARENT_DEVICE_EXT> and returns the result.
		964
		965	=item @device_partition_property_exts = $device->partition_types_ext
		966
		967	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_TYPES_EXT> and returns the result.
		968
		969	=item @device_partition_property_exts = $device->affinity_domains_ext
		970
		971	Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.
		972
		973	=item $uint = $device->reference_count_ext
		974
		975	Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT> and returns the result.
		976
		977	=item @device_partition_property_exts = $device->partition_style_ext
		978
		979	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_STYLE_EXT> and returns the result.
		980
		981	=for gengetinfo end device
		982
385	=back	983	=back
386		984
387	=head2 THE OpenCL::Context CLASS	985	=head2 THE OpenCL::Context CLASS
388		986
389	=over 4	987	=over 4
390		988
		989	=item $prog = $ctx->build_program ($program, $options = "")
		990
		991	This convenience function tries to build the program on all devices in
		992	the context. If the build fails, then the function will C<croak> with the
		993	build log. Otherwise ti returns the program object.
		994
		995	The C<$program> can either be a C<OpenCL::Program> object or a string
		996	containing the program. In the latter case, a program objetc will be
		997	created automatically.
		998
		999	=cut
		1000
		1001	sub OpenCL::Context::build_program {
		1002	my ($self, $prog, $options) = @_;
		1003
		1004	require Carp;
		1005
		1006	$prog = $self->program_with_source ($prog)
		1007	unless ref $prog;
		1008
		1009	# we build separately per device so we instantly know which one failed
		1010	for my $dev ($self->devices) {
		1011	eval { $prog->build ([$dev], $options); 1 }
		1012	or Carp::croak ("Building OpenCL program for device '" . $dev->name . "' failed:\n"
		1013	. $prog->build_log ($dev));
		1014	}
		1015
		1016	$prog
		1017	}
		1018
391	=item $queue = $ctx->queue ($device, $properties)	1019	=item $queue = $ctx->queue ($device, $properties)
392		1020
393	Create a new OpenCL::Queue object from the context and the given device.	1021	Create a new OpenCL::Queue object from the context and the given device.
394		1022
395	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html>	1023	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html>
396		1024
		1025	Example: create an out-of-order queue.
		1026
		1027	$queue = $ctx->queue ($device, OpenCL::QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE);
		1028
397	=item $ev = $ctx->user_event	1029	=item $ev = $ctx->user_event
398		1030
399	Creates a new OpenCL::UserEvent object.	1031	Creates a new OpenCL::UserEvent object.
400		1032
401	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateUserEvent.html>	1033	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateUserEvent.html>
402		1034
403	=item $buf = $ctx->buffer ($flags, $len)	1035	=item $buf = $ctx->buffer ($flags, $len)
404		1036
405	Creates a new OpenCL::Buffer object with the given flags and octet-size.	1037	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object with the
		1038	given flags and octet-size.
406		1039
407	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html>	1040	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html>
408		1041
409	=item $buf = $ctx->buffer_sv ($flags, $data)	1042	=item $buf = $ctx->buffer_sv ($flags, $data)
410		1043
411	Creates a new OpenCL::Buffer object and initialise it with the given data values.	1044	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and
		1045	initialise it with the given data values.
		1046
		1047	=item $img = $ctx->image ($self, $flags, $channel_order, $channel_type, $type, $width, $height, $depth, $array_size = 0, $row_pitch = 0, $slice_pitch = 0, $num_mip_level = 0, $num_samples = 0, $*data = &PL_sv_undef)
		1048
		1049	Creates a new OpenCL::Image object and optionally initialises it with
		1050	the given data values.
		1051
		1052	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateImage.html>
412		1053
413	=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)	1054	=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)
414		1055
415	Creates a new OpenCL::Image2D object and optionally initialises it with the given data values.	1056	Creates a new OpenCL::Image2D object and optionally initialises it with
		1057	the given data values.
416		1058
417	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage2D.html>	1059	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage2D.html>
418		1060
419	=item $img = $ctx->image3d ($flags, $channel_order, $channel_type, $width, $height, $depth, $row_pitch = 0, $slice_pitch = 0, $data = undef)	1061	=item $img = $ctx->image3d ($flags, $channel_order, $channel_type, $width, $height, $depth, $row_pitch = 0, $slice_pitch = 0, $data = undef)
420		1062
421	Creates a new OpenCL::Image3D object and optionally initialises it with the given data values.	1063	Creates a new OpenCL::Image3D object and optionally initialises it with
		1064	the given data values.
422		1065
423	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage3D.html>	1066	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage3D.html>
		1067
		1068	=item $buffer = $ctx->gl_buffer ($flags, $bufobj)
		1069
		1070	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given
		1071	OpenGL buffer object.
		1072
		1073	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html
		1074
		1075	=item $img = $ctx->gl_texture ($flags, $target, $miplevel, $texture)
		1076
		1077	Creates a new OpenCL::Image object that refers to the given OpenGL
		1078	texture object or buffer.
		1079
		1080	http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateFromGLTexture.html
		1081
		1082	=item $img = $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)
		1083
		1084	Creates a new OpenCL::Image2D object that refers to the given OpenGL
		1085	2D texture object.
		1086
		1087	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture2D.html
		1088
		1089	=item $img = $ctx->gl_texture3d ($flags, $target, $miplevel, $texture)
		1090
		1091	Creates a new OpenCL::Image3D object that refers to the given OpenGL
		1092	3D texture object.
		1093
		1094	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture3D.html
		1095
		1096	=item $ctx->gl_renderbuffer ($flags, $renderbuffer)
		1097
		1098	Creates a new OpenCL::Image2D object that refers to the given OpenGL
		1099	render buffer.
		1100
		1101	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLRenderbuffer.html
424		1102
425	=item @formats = $ctx->supported_image_formats ($flags, $image_type)	1103	=item @formats = $ctx->supported_image_formats ($flags, $image_type)
426		1104
427	Returns a list of matching image formats - each format is an arrayref with	1105	Returns a list of matching image formats - each format is an arrayref with
428	two values, $channel_order and $channel_type, in it.	1106	two values, $channel_order and $channel_type, in it.
…		…
446	See C<< $platform->info >> for details.	1124	See C<< $platform->info >> for details.
447		1125
448	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetContextInfo.html>	1126	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetContextInfo.html>
449		1127
450	=for gengetinfo begin context	1128	=for gengetinfo begin context
		1129
		1130	=item $uint = $context->reference_count
		1131
		1132	Calls C<clGetContextInfo> with C<CL_CONTEXT_REFERENCE_COUNT> and returns the result.
		1133
		1134	=item @devices = $context->devices
		1135
		1136	Calls C<clGetContextInfo> with C<CL_CONTEXT_DEVICES> and returns the result.
		1137
		1138	=item @property_ints = $context->properties
		1139
		1140	Calls C<clGetContextInfo> with C<CL_CONTEXT_PROPERTIES> and returns the result.
		1141
		1142	=item $uint = $context->num_devices
		1143
		1144	Calls C<clGetContextInfo> with C<CL_CONTEXT_NUM_DEVICES> and returns the result.
451		1145
452	=for gengetinfo end context	1146	=for gengetinfo end context
453		1147
454	=back	1148	=back
455		1149
…		…
463	for completion, unless the method is called in void context, in which case	1157	for completion, unless the method is called in void context, in which case
464	no event object is created.	1158	no event object is created.
465		1159
466	They also allow you to specify any number of other event objects that this	1160	They also allow you to specify any number of other event objects that this
467	request has to wait for before it starts executing, by simply passing the	1161	request has to wait for before it starts executing, by simply passing the
468	event objects as extra parameters to the enqueue methods.	1162	event objects as extra parameters to the enqueue methods. To simplify
		1163	program design, this module ignores any C<undef> values in the list of
		1164	events. This makes it possible to code operations such as this, without
		1165	having to put a valid event object into C<$event> first:
		1166
		1167	$event = $queue->enqueue_xxx (..., $event);
469		1168
470	Queues execute in-order by default, without any parallelism, so in most	1169	Queues execute in-order by default, without any parallelism, so in most
471	cases (i.e. you use only one queue) it's not necessary to wait for or	1170	cases (i.e. you use only one queue) it's not necessary to wait for or
472	create event objects.	1171	create event objects, althoguh an our of order queue is often a bit
		1172	faster.
473		1173
474	=over 4	1174	=over 4
475		1175
476	=item $packed_value = $ctx->info ($name)
477
478	See C<< $platform->info >> for details.
479
480	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetCommandQueueInfo.html>
481
482	=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...)	1176	=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...)
483		1177
484	Reads data from buffer into the given string.	1178	Reads data from buffer into the given string.
485		1179
486	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBuffer.html>	1180	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBuffer.html>
…		…
493		1187
494	=item $ev = $queue->enqueue_copy_buffer ($src, $dst, $src_offset, $dst_offset, $len, $wait_events...)	1188	=item $ev = $queue->enqueue_copy_buffer ($src, $dst, $src_offset, $dst_offset, $len, $wait_events...)
495		1189
496	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBuffer.html>	1190	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBuffer.html>
497		1191
		1192	=item $ev = $queue->enqueue_read_buffer_rect (OpenCL::Memory buf, cl_bool blocking, $buf_x, $buf_y, $buf_z, $host_x, $host_y, $host_z, $width, $height, $depth, $buf_row_pitch, $buf_slice_pitch, $host_row_pitch, $host_slice_pitch, $data, $wait_events...)
		1193
		1194	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBufferRect.html
		1195
		1196	=item $ev = $queue->enqueue_write_buffer_rect (OpenCL::Memory buf, cl_bool blocking, $buf_x, $buf_y, $buf_z, $host_x, $host_y, $host_z, $width, $height, $depth, $buf_row_pitch, $buf_slice_pitch, $host_row_pitch, $host_slice_pitch, $data, $wait_events...)
		1197
		1198	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteBufferRect.html
		1199
498	=item $ev = $queue->enqueue_read_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...)	1200	=item $ev = $queue->enqueue_read_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...)
499		1201
		1202	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferRect.html>
		1203
		1204	=item $ev = $queue->enqueue_copy_buffer_to_image ($src_buffer, $dst_image, $src_offset, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)
		1205
500	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadImage.html>	1206	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadImage.html>
501		1207
502	=item $ev = $queue->enqueue_write_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...)	1208	=item $ev = $queue->enqueue_write_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...)
503		1209
504	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteImage.html>	1210	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteImage.html>
505		1211
		1212	=item $ev = $queue->enqueue_copy_image ($src_image, $dst_image, $src_x, $src_y, $src_z, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)
		1213
		1214	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImage.html>
		1215
		1216	=item $ev = $queue->enqueue_copy_image_to_buffer ($src_image, $dst_image, $src_x, $src_y, $src_z, $width, $height, $depth, $dst_offset, $wait_events...)
		1217
		1218	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImageToBuffer.html>
		1219
506	=item $ev = $queue->enqueue_copy_buffer_rect ($src, $dst, $src_x, $src_y, $src_z, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $src_row_pitch, $src_slice_pitch, $dst_row_pitch, $dst_slice_pitch, $wait_event...)	1220	=item $ev = $queue->enqueue_copy_buffer_rect ($src, $dst, $src_x, $src_y, $src_z, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $src_row_pitch, $src_slice_pitch, $dst_row_pitch, $dst_slice_pitch, $wait_event...)
507		1221
508	Yeah.	1222	Yeah.
509		1223
510	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferRect.html>
511
512	=item $ev = $queue->enqueue_copy_buffer_to_image ($src_buffer, $dst_image, $src_offset, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)
513
514	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferToImage.html>.	1224	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferToImage.html>.
515		1225
516	=item $ev = $queue->enqueue_copy_image ($src_image, $dst_image, $src_x, $src_y, $src_z, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)	1226	=item $ev = $queue->enqueue_fill_buffer ($mem, $pattern, $offset, $size, ...)
517		1227
		1228	Fills the given buffer object with repeated applications of C<$pattern>,
		1229	starting at C<$offset> for C<$size> octets.
		1230
		1231	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueFillBuffer.html>
		1232
		1233	=item $ev = $queue->enqueue_fill_image ($img, $r, $g, $b, $a, $x, $y, $z, $width, $height, $depth, ...)
		1234
		1235	Fills the given image area with the given rgba colour components. The
		1236	components are normally floating point values between C<0> and C<1>,
		1237	except when the image channel data type is a signe dor unsigned
		1238	unnormalised format, in which case the range is determined by the format.
		1239
518	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImage.html>	1240	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueFillImage.html>
519
520	=item $ev = $queue->enqueue_copy_image_to_buffer ($src_image, $dst_image, $src_x, $src_y, $src_z, $width, $height, $depth, $dst_offset, $wait_events...)
521
522	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImageToBuffer.html>
523		1241
524	=item $ev = $queue->enqueue_task ($kernel, $wait_events...)	1242	=item $ev = $queue->enqueue_task ($kernel, $wait_events...)
525		1243
526	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueTask.html>	1244	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueTask.html>
527		1245
…		…
541	reference to an array of local work sizes, with the same number of	1259	reference to an array of local work sizes, with the same number of
542	elements as @$global_work_size.	1260	elements as @$global_work_size.
543		1261
544	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>	1262	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>
545		1263
546	=item $ev = $queue->enqueue_marker	1264	=item $ev = $queue->enqueue_acquire_gl_objects ([object, ...], $wait_events...)
547		1265
		1266	Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired
		1267	for subsequent OpenCL usage.
		1268
548	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMarker.html>	1269	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueAcquireGLObjects.html>
		1270
		1271	=item $ev = $queue->enqueue_release_gl_objects ([object, ...], $wait_events...)
		1272
		1273	Enqueues a list (an array-ref of OpenCL::Memory objects) to be released
		1274	for subsequent OpenGL usage.
		1275
		1276	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReleaseGLObjects.html>
549		1277
550	=item $ev = $queue->enqueue_wait_for_events ($wait_events...)	1278	=item $ev = $queue->enqueue_wait_for_events ($wait_events...)
551		1279
552	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWaitForEvents.html>	1280	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWaitForEvents.html>
553		1281
554	=item $queue->enqueue_barrier	1282	=item $ev = $queue->enqueue_marker ($wait_events...)
555		1283
		1284	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueMarkerWithWaitList.html>
		1285
		1286	=item $ev = $queue->enqueue_barrier ($wait_events...)
		1287
556	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueBarrier.html>	1288	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueBarrierWithWaitList.html>
557		1289
558	=item $queue->flush	1290	=item $queue->flush
559		1291
560	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFlush.html>	1292	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFlush.html>
561		1293
562	=item $queue->finish	1294	=item $queue->finish
563		1295
564	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFinish.html>	1296	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFinish.html>
565		1297
		1298	=item $packed_value = $queue->info ($name)
		1299
		1300	See C<< $platform->info >> for details.
		1301
		1302	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetCommandQueueInfo.html>
		1303
		1304	=for gengetinfo begin command_queue
		1305
		1306	=item $ctx = $command_queue->context
		1307
		1308	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_CONTEXT> and returns the result.
		1309
		1310	=item $device = $command_queue->device
		1311
		1312	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_DEVICE> and returns the result.
		1313
		1314	=item $uint = $command_queue->reference_count
		1315
		1316	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_REFERENCE_COUNT> and returns the result.
		1317
		1318	=item $command_queue_properties = $command_queue->properties
		1319
		1320	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_PROPERTIES> and returns the result.
		1321
		1322	=for gengetinfo end command_queue
		1323
566	=back	1324	=back
567		1325
568	=head2 THE OpenCL::Memory CLASS	1326	=head2 THE OpenCL::Memory CLASS
569		1327
570	This the superclass of all memory objects - OpenCL::Buffer, OpenCL::Image,	1328	This the superclass of all memory objects - OpenCL::Buffer, OpenCL::Image,
571	OpenCL::Image2D and OpenCL::Image3D. The subclasses of this class	1329	OpenCL::Image2D and OpenCL::Image3D.
572	currently only exist to allow type-checking.
573		1330
574	=over 4	1331	=over 4
575		1332
576	=item $packed_value = $memory->info ($name)	1333	=item $packed_value = $memory->info ($name)
577		1334
578	See C<< $platform->info >> for details.	1335	See C<< $platform->info >> for details.
579		1336
580	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetMemObjectInfo.html>	1337	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetMemObjectInfo.html>
581		1338
		1339	=for gengetinfo begin mem
		1340
		1341	=item $mem_object_type = $mem->type
		1342
		1343	Calls C<clGetMemObjectInfo> with C<CL_MEM_TYPE> and returns the result.
		1344
		1345	=item $mem_flags = $mem->flags
		1346
		1347	Calls C<clGetMemObjectInfo> with C<CL_MEM_FLAGS> and returns the result.
		1348
		1349	=item $int = $mem->size
		1350
		1351	Calls C<clGetMemObjectInfo> with C<CL_MEM_SIZE> and returns the result.
		1352
		1353	=item $ptr_value = $mem->host_ptr
		1354
		1355	Calls C<clGetMemObjectInfo> with C<CL_MEM_HOST_PTR> and returns the result.
		1356
		1357	=item $uint = $mem->map_count
		1358
		1359	Calls C<clGetMemObjectInfo> with C<CL_MEM_MAP_COUNT> and returns the result.
		1360
		1361	=item $uint = $mem->reference_count
		1362
		1363	Calls C<clGetMemObjectInfo> with C<CL_MEM_REFERENCE_COUNT> and returns the result.
		1364
		1365	=item $ctx = $mem->context
		1366
		1367	Calls C<clGetMemObjectInfo> with C<CL_MEM_CONTEXT> and returns the result.
		1368
		1369	=item $mem = $mem->associated_memobject
		1370
		1371	Calls C<clGetMemObjectInfo> with C<CL_MEM_ASSOCIATED_MEMOBJECT> and returns the result.
		1372
		1373	=item $int = $mem->offset
		1374
		1375	Calls C<clGetMemObjectInfo> with C<CL_MEM_OFFSET> and returns the result.
		1376
		1377	=for gengetinfo end mem
		1378
		1379	=item ($type, $name) = $mem->gl_object_info
		1380
		1381	Returns the OpenGL object type (e.g. OpenCL::GL_OBJECT_TEXTURE2D) and the
		1382	object "name" (e.g. the texture name) used to create this memory object.
		1383
		1384	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetGLObjectInfo.html>
		1385
582	=back	1386	=back
583		1387
		1388	=head2 THE OpenCL::Buffer CLASS
		1389
		1390	This is a subclass of OpenCL::Memory, and the superclass of
		1391	OpenCL::BufferObj. Its purpose is simply to distinguish between buffers
		1392	and sub-buffers.
		1393
		1394	=head2 THE OpenCL::BufferObj CLASS
		1395
		1396	This is a subclass of OpenCL::Buffer and thus OpenCL::Memory. It exists
		1397	because one cna create sub buffers of OpenLC::BufferObj objects, but not
		1398	sub buffers from these sub buffers.
		1399
		1400	=over 4
		1401
		1402	=item $subbuf = $buf_obj->sub_buffer_region ($flags, $origin, $size)
		1403
		1404	Creates an OpenCL::Buffer objects from this buffer and returns it. The
		1405	C<buffer_create_type> is assumed to be C<CL_BUFFER_CREATE_TYPE_REGION>.
		1406
		1407	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSubBuffer.html>
		1408
		1409	=back
		1410
584	=head2 THE OpenCL::Image CLASS	1411	=head2 THE OpenCL::Image CLASS
585		1412
586	This is the superclass of all image objects - OpenCL::Image2D and OpenCL::Image3D.	1413	This is the superclass of all image objects - OpenCL::Image1D,
		1414	OpenCL::Image1DArray, OpenCL::Image1DBuffer, OpenCL::Image2D,
		1415	OpenCL::Image2DArray and OpenCL::Image3D.
587		1416
588	=over 4	1417	=over 4
589		1418
590	=item $packed_value = $ev->image_info ($name)	1419	=item $packed_value = $image->image_info ($name)
591		1420
592	See C<< $platform->info >> for details.	1421	See C<< $platform->info >> for details.
593		1422
594	The reason this method is not called C<info> is that there already is an	1423	The reason this method is not called C<info> is that there already is an
595	C<< ->info >> method inherited from C<OpenCL::Memory>.	1424	C<< ->info >> method inherited from C<OpenCL::Memory>.
596		1425
597	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>	1426	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>
598		1427
		1428	=item ($channel_order, $channel_data_type) = $image->format
		1429
		1430	Returns the channel order and type used to create the image by calling
		1431	C<clGetImageInfo> with C<CL_IMAGE_FORMAT>.
		1432
		1433	=for gengetinfo begin image
		1434
		1435	=item $int = $image->element_size
		1436
		1437	Calls C<clGetImageInfo> with C<CL_IMAGE_ELEMENT_SIZE> and returns the result.
		1438
		1439	=item $int = $image->row_pitch
		1440
		1441	Calls C<clGetImageInfo> with C<CL_IMAGE_ROW_PITCH> and returns the result.
		1442
		1443	=item $int = $image->slice_pitch
		1444
		1445	Calls C<clGetImageInfo> with C<CL_IMAGE_SLICE_PITCH> and returns the result.
		1446
		1447	=item $int = $image->width
		1448
		1449	Calls C<clGetImageInfo> with C<CL_IMAGE_WIDTH> and returns the result.
		1450
		1451	=item $int = $image->height
		1452
		1453	Calls C<clGetImageInfo> with C<CL_IMAGE_HEIGHT> and returns the result.
		1454
		1455	=item $int = $image->depth
		1456
		1457	Calls C<clGetImageInfo> with C<CL_IMAGE_DEPTH> and returns the result.
		1458
		1459	=for gengetinfo end image
		1460
		1461	=for gengetinfo begin gl_texture
		1462
		1463	=item $GLenum = $gl_texture->target
		1464
		1465	Calls C<clGetGLTextureInfo> with C<CL_GL_TEXTURE_TARGET> and returns the result.
		1466
		1467	=item $GLint = $gl_texture->gl_mipmap_level
		1468
		1469	Calls C<clGetGLTextureInfo> with C<CL_GL_MIPMAP_LEVEL> and returns the result.
		1470
		1471	=for gengetinfo end gl_texture
		1472
599	=back	1473	=back
600		1474
601	=head2 THE OpenCL::Sampler CLASS	1475	=head2 THE OpenCL::Sampler CLASS
602		1476
603	=over 4	1477	=over 4
…		…
606		1480
607	See C<< $platform->info >> for details.	1481	See C<< $platform->info >> for details.
608		1482
609	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetSamplerInfo.html>	1483	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetSamplerInfo.html>
610		1484
		1485	=for gengetinfo begin sampler
		1486
		1487	=item $uint = $sampler->reference_count
		1488
		1489	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_REFERENCE_COUNT> and returns the result.
		1490
		1491	=item $ctx = $sampler->context
		1492
		1493	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_CONTEXT> and returns the result.
		1494
		1495	=item $addressing_mode = $sampler->normalized_coords
		1496
		1497	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_NORMALIZED_COORDS> and returns the result.
		1498
		1499	=item $filter_mode = $sampler->addressing_mode
		1500
		1501	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_ADDRESSING_MODE> and returns the result.
		1502
		1503	=item $boolean = $sampler->filter_mode
		1504
		1505	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_FILTER_MODE> and returns the result.
		1506
		1507	=for gengetinfo end sampler
		1508
611	=back	1509	=back
612		1510
613	=head2 THE OpenCL::Program CLASS	1511	=head2 THE OpenCL::Program CLASS
614		1512
615	=over 4	1513	=over 4
616		1514
617	=item $packed_value = $program->info ($name)	1515	=item $program->build (\@devices = undef, $options = "", $cb->($program) = undef)
618		1516
619	See C<< $platform->info >> for details.
620
621	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProgramInfo.html>
622
623	=item $program->build ($device, $options = "")
624
625	Tries to build the program with the givne options.	1517	Tries to build the program with the given options. See also the
		1518	C<$ctx->build> convenience function.
		1519
		1520	If a callback is specified, then it will be called when compilation is
		1521	finished. Note that many OpenCL implementations block your program while
		1522	compiling whether you use a callback or not. See C<build_async> if you
		1523	want to make sure the build is done in the background.
		1524
		1525	Note that some OpenCL implementations atc up badly, and don't call the
		1526	callback in some error cases (but call it in others). This implementation
		1527	assumes the callback will always be called, and leaks memory if this is
		1528	not so. So best make sure you don't pass in invalid values.
626		1529
627	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clBuildProgram.html>	1530	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clBuildProgram.html>
		1531
		1532	=item $program->build_async (\@devices = undef, $options = "", $cb->($program) = undef)
		1533
		1534	Similar to C<< ->build >>, except it starts a thread, and never fails (you
		1535	need to check the compilation status form the callback, or by polling).
628		1536
629	=item $packed_value = $program->build_info ($device, $name)	1537	=item $packed_value = $program->build_info ($device, $name)
630		1538
631	Similar to C<< $platform->info >>, but returns build info for a previous	1539	Similar to C<< $platform->info >>, but returns build info for a previous
632	build attempt for the given device.	1540	build attempt for the given device.
…		…
638	Creates an OpenCL::Kernel object out of the named C<__kernel> function in	1546	Creates an OpenCL::Kernel object out of the named C<__kernel> function in
639	the program.	1547	the program.
640		1548
641	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateKernel.html>	1549	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateKernel.html>
642		1550
		1551	=item @kernels = $program->kernels_in_program
		1552
		1553	Returns all kernels successfully compiled for all devices in program.
		1554
		1555	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateKernelsInProgram.html
		1556
		1557	=for gengetinfo begin program_build
		1558
		1559	=item $build_status = $program->build_status ($device)
		1560
		1561	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_STATUS> and returns the result.
		1562
		1563	=item $string = $program->build_options ($device)
		1564
		1565	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_OPTIONS> and returns the result.
		1566
		1567	=item $string = $program->build_log ($device)
		1568
		1569	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_LOG> and returns the result.
		1570
		1571	=for gengetinfo end program_build
		1572
		1573	=item $packed_value = $program->info ($name)
		1574
		1575	See C<< $platform->info >> for details.
		1576
		1577	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProgramInfo.html>
		1578
		1579	=for gengetinfo begin program
		1580
		1581	=item $uint = $program->reference_count
		1582
		1583	Calls C<clGetProgramInfo> with C<CL_PROGRAM_REFERENCE_COUNT> and returns the result.
		1584
		1585	=item $ctx = $program->context
		1586
		1587	Calls C<clGetProgramInfo> with C<CL_PROGRAM_CONTEXT> and returns the result.
		1588
		1589	=item $uint = $program->num_devices
		1590
		1591	Calls C<clGetProgramInfo> with C<CL_PROGRAM_NUM_DEVICES> and returns the result.
		1592
		1593	=item @devices = $program->devices
		1594
		1595	Calls C<clGetProgramInfo> with C<CL_PROGRAM_DEVICES> and returns the result.
		1596
		1597	=item $string = $program->source
		1598
		1599	Calls C<clGetProgramInfo> with C<CL_PROGRAM_SOURCE> and returns the result.
		1600
		1601	=item @ints = $program->binary_sizes
		1602
		1603	Calls C<clGetProgramInfo> with C<CL_PROGRAM_BINARY_SIZES> and returns the result.
		1604
		1605	=for gengetinfo end program
		1606
		1607	=item @blobs = $program->binaries
		1608
		1609	Returns a string for the compiled binary for every device associated with
		1610	the program, empty strings indicate missing programs, and an empty result
		1611	means no program binaries are available.
		1612
		1613	These "binaries" are often, in fact, informative low-level assembly
		1614	sources.
		1615
		1616	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProgramInfo.html>
		1617
643	=back	1618	=back
644		1619
645	=head2 THE OpenCL::Kernel CLASS	1620	=head2 THE OpenCL::Kernel CLASS
646		1621
647	=over 4	1622	=over 4
…		…
649	=item $packed_value = $kernel->info ($name)	1624	=item $packed_value = $kernel->info ($name)
650		1625
651	See C<< $platform->info >> for details.	1626	See C<< $platform->info >> for details.
652		1627
653	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelInfo.html>	1628	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelInfo.html>
		1629
		1630	=for gengetinfo begin kernel
		1631
		1632	=item $string = $kernel->function_name
		1633
		1634	Calls C<clGetKernelInfo> with C<CL_KERNEL_FUNCTION_NAME> and returns the result.
		1635
		1636	=item $uint = $kernel->num_args
		1637
		1638	Calls C<clGetKernelInfo> with C<CL_KERNEL_NUM_ARGS> and returns the result.
		1639
		1640	=item $uint = $kernel->reference_count
		1641
		1642	Calls C<clGetKernelInfo> with C<CL_KERNEL_REFERENCE_COUNT> and returns the result.
		1643
		1644	=item $ctx = $kernel->context
		1645
		1646	Calls C<clGetKernelInfo> with C<CL_KERNEL_CONTEXT> and returns the result.
		1647
		1648	=item $program = $kernel->program
		1649
		1650	Calls C<clGetKernelInfo> with C<CL_KERNEL_PROGRAM> and returns the result.
		1651
		1652	=for gengetinfo end kernel
654		1653
655	=item $packed_value = $kernel->work_group_info ($device, $name)	1654	=item $packed_value = $kernel->work_group_info ($device, $name)
656		1655
657	See C<< $platform->info >> for details.	1656	See C<< $platform->info >> for details.
658		1657
659	The reason this method is not called C<info> is that there already is an	1658	The reason this method is not called C<info> is that there already is an
660	C<< ->info >> method.	1659	C<< ->info >> method.
661		1660
662	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelWorkGroupInfo.html>	1661	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelWorkGroupInfo.html>
663		1662
		1663	=for gengetinfo begin kernel_work_group
		1664
		1665	=item $int = $kernel->work_group_size ($device)
		1666
		1667	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_WORK_GROUP_SIZE> and returns the result.
		1668
		1669	=item @ints = $kernel->compile_work_group_size ($device)
		1670
		1671	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_COMPILE_WORK_GROUP_SIZE> and returns the result.
		1672
		1673	=item $ulong = $kernel->local_mem_size ($device)
		1674
		1675	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_LOCAL_MEM_SIZE> and returns the result.
		1676
		1677	=item $int = $kernel->preferred_work_group_size_multiple ($device)
		1678
		1679	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE> and returns the result.
		1680
		1681	=item $ulong = $kernel->private_mem_size ($device)
		1682
		1683	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PRIVATE_MEM_SIZE> and returns the result.
		1684
		1685	=for gengetinfo end kernel_work_group
		1686
664	=item $kernel->set_TYPE ($index, $value)	1687	=item $kernel->set_TYPE ($index, $value)
665		1688
666	This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>.	1689	This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>.
667		1690
668	TYPE is one of C<char>, C<uchar>, C<short>, C<ushort>, C<int>, C<uint>,	1691	TYPE is one of C<char>, C<uchar>, C<short>, C<ushort>, C<int>, C<uint>,
669	C<long>, C<ulong>, C<half>, C<float>, C<double>, C<memory>, C<buffer>,	1692	C<long>, C<ulong>, C<half>, C<float>, C<double>, C<memory>, C<buffer>,
670	C<image2d>, C<image3d>, C<sampler> or C<event>.	1693	C<image2d>, C<image3d>, C<sampler>, C<local> or C<event>.
671		1694
672	Chars and integers (including the half type) are specified as integers,	1695	Chars and integers (including the half type) are specified as integers,
673	float and double as floating point values, memory/buffer/image2d/image3d	1696	float and double as floating point values, memory/buffer/image2d/image3d
674	must be an object of that type or C<undef>, and sampler and event must be	1697	must be an object of that type or C<undef>, local-memory arguments are
675	objects of that type.	1698	set by specifying the size, and sampler and event must be objects of that
		1699	type.
		1700
		1701	Setting an argument for a kernel does NOT keep a reference to the object -
		1702	for example, if you set an argument to some image object, free the image,
		1703	and call the kernel, you will run into undefined behaviour.
676		1704
677	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetKernelArg.html>	1705	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetKernelArg.html>
678		1706
679	=back	1707	=back
680		1708
…		…
683	This is the superclass for all event objects (including OpenCL::UserEvent	1711	This is the superclass for all event objects (including OpenCL::UserEvent
684	objects).	1712	objects).
685		1713
686	=over 4	1714	=over 4
687		1715
		1716	=item $ev->wait
		1717
		1718	Waits for the event to complete.
		1719
		1720	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clWaitForEvents.html>
		1721
		1722	=item $ev->cb ($exec_callback_type, $callback->($event, $event_command_exec_status))
		1723
		1724	Adds a callback to the callback stack for the given event type. There is
		1725	no way to remove a callback again.
		1726
		1727	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetEventCallback.html>
		1728
688	=item $packed_value = $ev->info ($name)	1729	=item $packed_value = $ev->info ($name)
689		1730
690	See C<< $platform->info >> for details.	1731	See C<< $platform->info >> for details.
691		1732
692	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetEventInfo.html>	1733	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetEventInfo.html>
		1734
		1735	=for gengetinfo begin event
		1736
		1737	=item $queue = $event->command_queue
		1738
		1739	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_QUEUE> and returns the result.
		1740
		1741	=item $command_type = $event->command_type
		1742
		1743	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_TYPE> and returns the result.
		1744
		1745	=item $uint = $event->reference_count
		1746
		1747	Calls C<clGetEventInfo> with C<CL_EVENT_REFERENCE_COUNT> and returns the result.
		1748
		1749	=item $uint = $event->command_execution_status
		1750
		1751	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_EXECUTION_STATUS> and returns the result.
		1752
		1753	=item $ctx = $event->context
		1754
		1755	Calls C<clGetEventInfo> with C<CL_EVENT_CONTEXT> and returns the result.
		1756
		1757	=for gengetinfo end event
693		1758
694	=item $packed_value = $ev->profiling_info ($name)	1759	=item $packed_value = $ev->profiling_info ($name)
695		1760
696	See C<< $platform->info >> for details.	1761	See C<< $platform->info >> for details.
697		1762
698	The reason this method is not called C<info> is that there already is an	1763	The reason this method is not called C<info> is that there already is an
699	C<< ->info >> method.	1764	C<< ->info >> method.
700		1765
701	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProfilingInfo.html>	1766	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProfilingInfo.html>
702		1767
703	=item $ev->wait	1768	=for gengetinfo begin profiling
704		1769
705	Waits for the event to complete.	1770	=item $ulong = $event->profiling_command_queued
706		1771
707	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clWaitForEvents.html>	1772	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_QUEUED> and returns the result.
		1773
		1774	=item $ulong = $event->profiling_command_submit
		1775
		1776	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_SUBMIT> and returns the result.
		1777
		1778	=item $ulong = $event->profiling_command_start
		1779
		1780	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_START> and returns the result.
		1781
		1782	=item $ulong = $event->profiling_command_end
		1783
		1784	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_END> and returns the result.
		1785
		1786	=for gengetinfo end profiling
708		1787
709	=back	1788	=back
710		1789
711	=head2 THE OpenCL::UserEvent CLASS	1790	=head2 THE OpenCL::UserEvent CLASS
712		1791
…		…
714		1793
715	=over 4	1794	=over 4
716		1795
717	=item $ev->set_status ($execution_status)	1796	=item $ev->set_status ($execution_status)
718		1797
		1798	Sets the execution status of the user event. Can only be called once,
		1799	either with OpenCL::COMPLETE or a negative number as status.
		1800
719	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetUserEventStatus.html>	1801	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetUserEventStatus.html>
720		1802
721	=back	1803	=back
722		1804
723	=cut	1805	=cut
724
725	package OpenCL;
726
727	use common::sense;
728
729	BEGIN {
730	our $VERSION = '0.15';
731
732	require XSLoader;
733	XSLoader::load (__PACKAGE__, $VERSION);
734
735	@OpenCL::Buffer::ISA =
736	@OpenCL::Image::ISA = OpenCL::Memory::;
737
738	@OpenCL::Image2D::ISA =
739	@OpenCL::Image3D::ISA = OpenCL::Image::;
740
741	@OpenCL::UserEvent::ISA = OpenCL::Event::;
742	}
743		1806
744	1;	1807	1;
745		1808
746	=head1 AUTHOR	1809	=head1 AUTHOR
747		1810

Diff Legend

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