[ViewVC] Diff of: cvs/OpenCL/OpenCL.pm

Comparing OpenCL/OpenCL.pm (file contents):
Revision 1.32 by root, Thu Apr 19 12:12:03 2012 UTC vs.
Revision 1.53 by root, Tue Apr 24 14:30:57 2012 UTC

…		…
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_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
276	=head2 OpenGL sharing	366	=head2 GLX SUPPORT
277		367
278	This module can be optionally compiled with support for	368	Due to the sad state that OpenGL support is in in Perl (mostly the OpenGL
279	OpenGL sharing. The sharing functions are only available when	369	module, which has little to no documentation and has little to no support
280	C<OpenCL::HAVE_OPENGL> returns true, otherwise they are absent and cannot	370	for glX), this module, as a special extension, treats context creation
281	be called.	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	=cut
		382
		383	package OpenCL;
		384
		385	use common::sense;
		386
		387	BEGIN {
		388	our $VERSION = '0.96';
		389
		390	require XSLoader;
		391	XSLoader::load (__PACKAGE__, $VERSION);
		392
		393	@OpenCL::Platform::ISA =
		394	@OpenCL::Device::ISA =
		395	@OpenCL::Context::ISA =
		396	@OpenCL::Queue::ISA =
		397	@OpenCL::Memory::ISA =
		398	@OpenCL::Sampler::ISA =
		399	@OpenCL::Program::ISA =
		400	@OpenCL::Kernel::ISA =
		401	@OpenCL::Event::ISA = OpenCL::Object::;
		402
		403	@OpenCL::Buffer::ISA =
		404	@OpenCL::Image::ISA = OpenCL::Memory::;
		405
		406	@OpenCL::BufferObj::ISA = OpenCL::Buffer::;
		407
		408	@OpenCL::Image2D::ISA =
		409	@OpenCL::Image3D::ISA =
		410	@OpenCL::Image2DArray::ISA =
		411	@OpenCL::Image1D::ISA =
		412	@OpenCL::Image1DArray::ISA =
		413	@OpenCL::Image1DBuffer::ISA = OpenCL::Image::;
		414
		415	@OpenCL::UserEvent::ISA = OpenCL::Event::;
		416	}
282		417
283	=head2 THE OpenCL PACKAGE	418	=head2 THE OpenCL PACKAGE
284		419
285	=over 4	420	=over 4
286		421
…		…
319		454
320	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clWaitForEvents.html>	455	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clWaitForEvents.html>
321		456
322	=back	457	=back
323		458
		459	=head2 THE OpenCL::Object CLASS
		460
		461	This is the base class for all objects in the OpenCL module. The only
		462	method it implements is the C<id> method, which is only useful if you want
		463	to interface to OpenCL on the C level.
		464
		465	=over 4
		466
		467	=item $iv = $obj->id
		468
		469	OpenCL objects are represented by pointers or integers on the C level. If
		470	you want to interface to an OpenCL object directly on the C level, then
		471	you need this value, which is returned by this method. You should use an
		472	C<IV> type in your code and cast that to the correct type.
		473
		474	=cut
		475
		476	sub OpenCL::Object::id {
		477	${$_[0]}
		478	}
		479
		480	=back
		481
324	=head2 THE OpenCL::Platform CLASS	482	=head2 THE OpenCL::Platform CLASS
325		483
326	=over 4	484	=over 4
327		485
328	=item @devices = $platform->devices ($type = OpenCL::DEVICE_TYPE_ALL)	486	=item @devices = $platform->devices ($type = OpenCL::DEVICE_TYPE_ALL)
…		…
351	It's best to avoid this method and use one of the following convenience	509	It's best to avoid this method and use one of the following convenience
352	wrappers.	510	wrappers.
353		511
354	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformInfo.html>	512	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformInfo.html>
355		513
		514	=item $platform->unload_compiler
		515
		516	Attempts to unload the compiler for this platform, for endless
		517	profit. Does nothing on OpenCL 1.1.
		518
		519	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clUnloadPlatformCompiler.html>
		520
356	=for gengetinfo begin platform	521	=for gengetinfo begin platform
357		522
358	=item $string = $platform->profile	523	=item $string = $platform->profile
359		524
360	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result.	525	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result.
…		…
645		810
646	=item @device_partition_property_exts = $device->affinity_domains_ext	811	=item @device_partition_property_exts = $device->affinity_domains_ext
647		812
648	Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.	813	Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.
649		814
650	=item $uint = $device->reference_count_ext	815	=item $uint = $device->reference_count_ext
651		816
652	Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT > and returns the result.	817	Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT> and returns the result.
653		818
654	=item @device_partition_property_exts = $device->partition_style_ext	819	=item @device_partition_property_exts = $device->partition_style_ext
655		820
656	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_STYLE_EXT> and returns the result.	821	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_STYLE_EXT> and returns the result.
657		822
…		…
661		826
662	=head2 THE OpenCL::Context CLASS	827	=head2 THE OpenCL::Context CLASS
663		828
664	=over 4	829	=over 4
665		830
		831	=item $prog = $ctx->build_program ($program, $options = "")
		832
		833	This convenience function tries to build the program on all devices in
		834	the context. If the build fails, then the function will C<croak> with the
		835	build log. Otherwise ti returns the program object.
		836
		837	The C<$program> can either be a C<OpenCL::Program> object or a string
		838	containing the program. In the latter case, a program objetc will be
		839	created automatically.
		840
		841	=cut
		842
		843	sub OpenCL::Context::build_program {
		844	my ($self, $prog, $options) = @_;
		845
		846	$prog = $self->program_with_source ($prog)
		847	unless ref $prog;
		848
		849	for my $dev ($self->devices) {
		850	eval { $prog->build ($dev, $options); 1 }
		851	or Carp::croak "Building OpenCL program for device '" . $dev->name . "' failed:\n"
		852	. $prog->build_log ($dev);
		853	}
		854
		855	$prog
		856	}
		857
666	=item $queue = $ctx->queue ($device, $properties)	858	=item $queue = $ctx->queue ($device, $properties)
667		859
668	Create a new OpenCL::Queue object from the context and the given device.	860	Create a new OpenCL::Queue object from the context and the given device.
669		861
670	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html>	862	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html>
		863
		864	Example: create an out-of-order queue.
		865
		866	$queue = $ctx->queue ($device, OpenCL::QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE);
671		867
672	=item $ev = $ctx->user_event	868	=item $ev = $ctx->user_event
673		869
674	Creates a new OpenCL::UserEvent object.	870	Creates a new OpenCL::UserEvent object.
675		871
…		…
685	=item $buf = $ctx->buffer_sv ($flags, $data)	881	=item $buf = $ctx->buffer_sv ($flags, $data)
686		882
687	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and	883	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and
688	initialise it with the given data values.	884	initialise it with the given data values.
689		885
		886	=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)
		887
		888	Creates a new OpenCL::Image object and optionally initialises it with
		889	the given data values.
		890
		891	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateImage.html>
		892
690	=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)	893	=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)
691		894
692	Creates a new OpenCL::Image2D object and optionally initialises it with	895	Creates a new OpenCL::Image2D object and optionally initialises it with
693	the given data values.	896	the given data values.
694		897
…		…
698		901
699	Creates a new OpenCL::Image3D object and optionally initialises it with	902	Creates a new OpenCL::Image3D object and optionally initialises it with
700	the given data values.	903	the given data values.
701		904
702	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage3D.html>	905	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage3D.html>
		906
		907	=item $buffer = $ctx->gl_buffer ($flags, $bufobj)
		908
		909	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given
		910	OpenGL buffer object.
		911
		912	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html
		913
		914	=item $img = $ctx->gl_texture ($flags, $target, $miplevel, $texture)
		915
		916	Creates a new OpenCL::Image object that refers to the given OpenGL
		917	texture object or buffer.
		918
		919	http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateFromGLTexture.html
		920
		921	=item $img = $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)
		922
		923	Creates a new OpenCL::Image2D object that refers to the given OpenGL
		924	2D texture object.
		925
		926	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture2D.html
		927
		928	=item $img = $ctx->gl_texture3d ($flags, $target, $miplevel, $texture)
		929
		930	Creates a new OpenCL::Image3D object that refers to the given OpenGL
		931	3D texture object.
		932
		933	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture3D.html
		934
		935	=item $ctx->gl_renderbuffer ($flags, $renderbuffer)
		936
		937	Creates a new OpenCL::Image2D object that refers to the given OpenGL
		938	render buffer.
		939
		940	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLRenderbuffer.html
703		941
704	=item @formats = $ctx->supported_image_formats ($flags, $image_type)	942	=item @formats = $ctx->supported_image_formats ($flags, $image_type)
705		943
706	Returns a list of matching image formats - each format is an arrayref with	944	Returns a list of matching image formats - each format is an arrayref with
707	two values, $channel_order and $channel_type, in it.	945	two values, $channel_order and $channel_type, in it.
…		…
758	for completion, unless the method is called in void context, in which case	996	for completion, unless the method is called in void context, in which case
759	no event object is created.	997	no event object is created.
760		998
761	They also allow you to specify any number of other event objects that this	999	They also allow you to specify any number of other event objects that this
762	request has to wait for before it starts executing, by simply passing the	1000	request has to wait for before it starts executing, by simply passing the
763	event objects as extra parameters to the enqueue methods.	1001	event objects as extra parameters to the enqueue methods. To simplify
		1002	program design, this module ignores any C<undef> values in the list of
		1003	events. This makes it possible to code operations such as this, without
		1004	having to put a valid event object into C<$event> first:
		1005
		1006	$event = $queue->enqueue_xxx (..., $event);
764		1007
765	Queues execute in-order by default, without any parallelism, so in most	1008	Queues execute in-order by default, without any parallelism, so in most
766	cases (i.e. you use only one queue) it's not necessary to wait for or	1009	cases (i.e. you use only one queue) it's not necessary to wait for or
767	create event objects.	1010	create event objects, althoguh an our of order queue is often a bit
		1011	faster.
768		1012
769	=over 4	1013	=over 4
770		1014
771	=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...)	1015	=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...)
772		1016
…		…
815	=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...)	1059	=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...)
816		1060
817	Yeah.	1061	Yeah.
818		1062
819	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferToImage.html>.	1063	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferToImage.html>.
		1064
		1065	=item $ev = $queue->enqueue_fill_buffer ($mem, $pattern, $offset, $size, ...)
		1066
		1067	Fills the given buffer object with repeated applications of C<$pattern>,
		1068	starting at C<$offset> for C<$size> octets.
		1069
		1070	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueFillBuffer.html>
		1071
		1072	=item $ev = $queue->enqueue_fill_image ($img, $r, $g, $b, $a, $x, $y, $z, $width, $height, $depth, ...)
		1073
		1074	Fills the given image area with the given rgba colour components. The
		1075	components are normally floating point values between C<0> and C<1>,
		1076	except when the image channel data type is a signe dor unsigned
		1077	unnormalised format, in which case the range is determined by the format.
		1078
		1079	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueFillImage.html>
820		1080
821	=item $ev = $queue->enqueue_task ($kernel, $wait_events...)	1081	=item $ev = $queue->enqueue_task ($kernel, $wait_events...)
822		1082
823	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueTask.html>	1083	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueTask.html>
824		1084
…		…
838	reference to an array of local work sizes, with the same number of	1098	reference to an array of local work sizes, with the same number of
839	elements as @$global_work_size.	1099	elements as @$global_work_size.
840		1100
841	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>	1101	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>
842		1102
843	=item $ev = $queue->enqueue_marker	1103	=item $ev = $queue->enqueue_acquire_gl_objects ([object, ...], $wait_events...)
844		1104
		1105	Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired
		1106	for subsequent OpenCL usage.
		1107
845	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMarker.html>	1108	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueAcquireGLObjects.html>
		1109
		1110	=item $ev = $queue->enqueue_release_gl_objects ([object, ...], $wait_events...)
		1111
		1112	Enqueues a list (an array-ref of OpenCL::Memory objects) to be released
		1113	for subsequent OpenGL usage.
		1114
		1115	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReleaseGLObjects.html>
846		1116
847	=item $ev = $queue->enqueue_wait_for_events ($wait_events...)	1117	=item $ev = $queue->enqueue_wait_for_events ($wait_events...)
848		1118
849	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWaitForEvents.html>	1119	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWaitForEvents.html>
850		1120
851	=item $queue->enqueue_barrier	1121	=item $ev = $queue->enqueue_marker ($wait_events...)
852		1122
		1123	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueMarkerWithWaitList.html>
		1124
		1125	=item $ev = $queue->enqueue_barrier ($wait_events...)
		1126
853	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueBarrier.html>	1127	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueBarrierWithWaitList.html>
854		1128
855	=item $queue->flush	1129	=item $queue->flush
856		1130
857	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFlush.html>	1131	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFlush.html>
858		1132
…		…
938	=item $int = $mem->offset	1212	=item $int = $mem->offset
939		1213
940	Calls C<clGetMemObjectInfo> with C<CL_MEM_OFFSET> and returns the result.	1214	Calls C<clGetMemObjectInfo> with C<CL_MEM_OFFSET> and returns the result.
941		1215
942	=for gengetinfo end mem	1216	=for gengetinfo end mem
		1217
		1218	=item ($type, $name) = $mem->gl_object_info
		1219
		1220	Returns the OpenGL object type (e.g. OpenCL::GL_OBJECT_TEXTURE2D) and the
		1221	object "name" (e.g. the texture name) used to create this memory object.
		1222
		1223	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetGLObjectInfo.html>
943		1224
944	=back	1225	=back
945		1226
946	=head2 THE OpenCL::Buffer CLASS	1227	=head2 THE OpenCL::Buffer CLASS
947		1228
…		…
966		1247
967	=back	1248	=back
968		1249
969	=head2 THE OpenCL::Image CLASS	1250	=head2 THE OpenCL::Image CLASS
970		1251
971	This is the superclass of all image objects - OpenCL::Image2D and OpenCL::Image3D.	1252	This is the superclass of all image objects - OpenCL::Image1D,
		1253	OpenCL::Image1DArray, OpenCL::Image1DBuffer, OpenCL::Image2D,
		1254	OpenCL::Image2DArray and OpenCL::Image3D.
972		1255
973	=over 4	1256	=over 4
974		1257
975	=item $packed_value = $ev->image_info ($name)	1258	=item $packed_value = $image->image_info ($name)
976		1259
977	See C<< $platform->info >> for details.	1260	See C<< $platform->info >> for details.
978		1261
979	The reason this method is not called C<info> is that there already is an	1262	The reason this method is not called C<info> is that there already is an
980	C<< ->info >> method inherited from C<OpenCL::Memory>.	1263	C<< ->info >> method inherited from C<OpenCL::Memory>.
981		1264
982	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>	1265	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>
983		1266
		1267	=item ($channel_order, $channel_data_type) = $image->format
		1268
		1269	Returns the channel order and type used to create the image by calling
		1270	C<clGetImageInfo> with C<CL_IMAGE_FORMAT>.
		1271
984	=for gengetinfo begin image	1272	=for gengetinfo begin image
985		1273
986	=item $int = $image->element_size	1274	=item $int = $image->element_size
987		1275
988	Calls C<clGetImageInfo> with C<CL_IMAGE_ELEMENT_SIZE> and returns the result.	1276	Calls C<clGetImageInfo> with C<CL_IMAGE_ELEMENT_SIZE> and returns the result.
…		…
1007		1295
1008	Calls C<clGetImageInfo> with C<CL_IMAGE_DEPTH> and returns the result.	1296	Calls C<clGetImageInfo> with C<CL_IMAGE_DEPTH> and returns the result.
1009		1297
1010	=for gengetinfo end image	1298	=for gengetinfo end image
1011		1299
		1300	=for gengetinfo begin gl_texture
		1301
		1302	=item $GLenum = $gl_texture->target
		1303
		1304	Calls C<clGetGLTextureInfo> with C<CL_GL_TEXTURE_TARGET> and returns the result.
		1305
		1306	=item $GLint = $gl_texture->gl_mipmap_level
		1307
		1308	Calls C<clGetGLTextureInfo> with C<CL_GL_MIPMAP_LEVEL> and returns the result.
		1309
		1310	=for gengetinfo end gl_texture
		1311
1012	=back	1312	=back
1013		1313
1014	=head2 THE OpenCL::Sampler CLASS	1314	=head2 THE OpenCL::Sampler CLASS
1015		1315
1016	=over 4	1316	=over 4
…		…
1051		1351
1052	=over 4	1352	=over 4
1053		1353
1054	=item $program->build ($device, $options = "")	1354	=item $program->build ($device, $options = "")
1055		1355
1056	Tries to build the program with the givne options.	1356	Tries to build the program with the given options. See also the
		1357	C<$ctx->build> convenience function.
1057		1358
1058	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clBuildProgram.html>	1359	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clBuildProgram.html>
1059		1360
1060	=item $packed_value = $program->build_info ($device, $name)	1361	=item $packed_value = $program->build_info ($device, $name)
1061		1362
…		…
1068		1369
1069	Creates an OpenCL::Kernel object out of the named C<__kernel> function in	1370	Creates an OpenCL::Kernel object out of the named C<__kernel> function in
1070	the program.	1371	the program.
1071		1372
1072	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateKernel.html>	1373	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateKernel.html>
		1374
		1375	=item @kernels = $program->kernels_in_program
		1376
		1377	Returns all kernels successfully compiled for all devices in program.
		1378
		1379	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateKernelsInProgram.html
1073		1380
1074	=for gengetinfo begin program_build	1381	=for gengetinfo begin program_build
1075		1382
1076	=item $build_status = $program->build_status ($device)	1383	=item $build_status = $program->build_status ($device)
1077		1384
…		…
1205		1512
1206	This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>.	1513	This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>.
1207		1514
1208	TYPE is one of C<char>, C<uchar>, C<short>, C<ushort>, C<int>, C<uint>,	1515	TYPE is one of C<char>, C<uchar>, C<short>, C<ushort>, C<int>, C<uint>,
1209	C<long>, C<ulong>, C<half>, C<float>, C<double>, C<memory>, C<buffer>,	1516	C<long>, C<ulong>, C<half>, C<float>, C<double>, C<memory>, C<buffer>,
1210	C<image2d>, C<image3d>, C<sampler> or C<event>.	1517	C<image2d>, C<image3d>, C<sampler>, C<local> or C<event>.
1211		1518
1212	Chars and integers (including the half type) are specified as integers,	1519	Chars and integers (including the half type) are specified as integers,
1213	float and double as floating point values, memory/buffer/image2d/image3d	1520	float and double as floating point values, memory/buffer/image2d/image3d
1214	must be an object of that type or C<undef>, and sampler and event must be	1521	must be an object of that type or C<undef>, local-memory arguments are
1215	objects of that type.	1522	set by specifying the size, and sampler and event must be objects of that
		1523	type.
		1524
		1525	Setting an argument for a kernel does NOT keep a reference to the object -
		1526	for example, if you set an argument to some image object, free the image,
		1527	and call the kernel, you will run into undefined behaviour.
1216		1528
1217	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetKernelArg.html>	1529	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetKernelArg.html>
1218		1530
1219	=back	1531	=back
1220		1532
…		…
1304		1616
1305	=back	1617	=back
1306		1618
1307	=cut	1619	=cut
1308		1620
1309	package OpenCL;
1310
1311	use common::sense;
1312
1313	BEGIN {
1314	our $VERSION = '0.92';
1315
1316	require XSLoader;
1317	XSLoader::load (__PACKAGE__, $VERSION);
1318
1319	@OpenCL::Buffer::ISA =
1320	@OpenCL::Image::ISA = OpenCL::Memory::;
1321
1322	@OpenCL::BufferObj::ISA = OpenCL::Buffer::;
1323
1324	@OpenCL::Image2D::ISA =
1325	@OpenCL::Image3D::ISA = OpenCL::Image::;
1326
1327	@OpenCL::UserEvent::ISA = OpenCL::Event::;
1328	}
1329
1330	1;	1621	1;
1331		1622
1332	=head1 AUTHOR	1623	=head1 AUTHOR
1333		1624
1334	Marc Lehmann <schmorp@schmorp.de>	1625	Marc Lehmann <schmorp@schmorp.de>

Diff Legend

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

Comparing OpenCL/OpenCL.pm (file contents): Revision 1.32 by root, Thu Apr 19 12:12:03 2012 UTC vs. Revision 1.53 by root, Tue Apr 24 14:30:57 2012 UTC

Diff Legend

Comparing OpenCL/OpenCL.pm (file contents):
Revision 1.32 by root, Thu Apr 19 12:12:03 2012 UTC vs.
Revision 1.53 by root, Tue Apr 24 14:30:57 2012 UTC