ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/OpenCL/OpenCL.xs

Comparing OpenCL/OpenCL.xs (file contents):
Revision 1.1 by root, Tue Nov 15 06:50:30 2011 UTC vs.
Revision 1.15 by root, Sun Nov 20 22:29:36 2011 UTC

…		…
6		6
7	typedef cl_platform_id OpenCL__Platform;	7	typedef cl_platform_id OpenCL__Platform;
8	typedef cl_device_id OpenCL__Device;	8	typedef cl_device_id OpenCL__Device;
9	typedef cl_context OpenCL__Context;	9	typedef cl_context OpenCL__Context;
10	typedef cl_command_queue OpenCL__Queue;	10	typedef cl_command_queue OpenCL__Queue;
		11	typedef cl_mem OpenCL__Memory;
		12	typedef cl_mem OpenCL__Buffer;
		13	typedef cl_mem OpenCL__Image;
		14	typedef cl_mem OpenCL__Image2D;
		15	typedef cl_mem OpenCL__Image3D;
		16	typedef cl_mem OpenCL__Memory_ornull;
		17	typedef cl_mem OpenCL__Buffer_ornull;
		18	typedef cl_mem OpenCL__Image_ornull;
		19	typedef cl_mem OpenCL__Image2D_ornull;
		20	typedef cl_mem OpenCL__Image3D_ornull;
		21	typedef cl_sampler OpenCL__Sampler;
		22	typedef cl_program OpenCL__Program;
		23	typedef cl_kernel OpenCL__Kernel;
		24	typedef cl_event OpenCL__Event;
		25	typedef cl_event OpenCL__UserEvent;
11		26
12	static const struct {	27	typedef SV *FUTURE;
		28
		29	/*****************************************************************************/
		30
		31	/* up to two temporary buffers */
		32	static void *
		33	tmpbuf (size_t size)
		34	{
		35	static int idx;
		36	static void *buf [2];
		37	static size_t len [2];
		38
		39	idx ^= 1;
		40
		41	if (len [idx] < size)
		42	{
		43	free (buf [idx]);
		44	len [idx] = ((size + 31) & ~4095) + 4096 - 32;
		45	buf [idx] = malloc (len [idx]);
		46	}
		47
		48	return buf [idx];
		49	}
		50
		51	/*****************************************************************************/
		52
		53	typedef struct
		54	{
13	IV iv;	55	IV iv;
14	const char *name;	56	const char *name;
15	} cl_error[] = {
16	#define def_error(name) { (IV)CL_ ## name, # name },	57	#define const_iv(name) { (IV)CL_ ## name, # name },
17	#include "invalid.h"	58	} ivstr;
18	};
19		59
20	static const char *	60	static const char *
21	clstrerror (cl_int res)	61	iv2str (IV value, const ivstr *base, int count, const char *fallback)
22	{	62	{
23	int i;	63	int i;
24	static char numbuf [32];	64	static char strbuf [32];
25		65
26	for (i = sizeof (cl_error) / sizeof (cl_error [0]); i--; )	66	for (i = count; i--; )
27	if (cl_error [i].iv == res)	67	if (base [i].iv == value)
28	return cl_error [i].name;	68	return base [i].name;
29		69
30	snprintf (numbuf, sizeof (numbuf), "ERROR(%d)", res);	70	snprintf (strbuf, sizeof (strbuf), fallback, (int)value);
31		71
32	return numbuf;	72	return strbuf;
33	}	73	}
34		74
		75	static const char *
		76	enum2str (cl_uint value)
		77	{
		78	static const ivstr enumstr[] = {
		79	#include "enumstr.h"
		80	};
		81
		82	return iv2str (value, enumstr, sizeof (enumstr) / sizeof (enumstr [0]), "ENUM(0x%04x)");
		83	}
		84
		85	static const char *
		86	err2str (cl_int err)
		87	{
		88	static const ivstr errstr[] = {
		89	#include "errstr.h"
		90	};
		91
		92	return iv2str (err, errstr, sizeof (errstr) / sizeof (errstr [0]), "ERROR(%d)");
		93	}
		94
		95	/*****************************************************************************/
		96
		97	static cl_int res;
		98
35	#define FAIL(name,res) \	99	#define FAIL(name) \
36	croak (# name ": %s", clstrerror (res));	100	croak ("cl" # name ": %s", err2str (res));
37		101
38	#define NEED_SUCCESS(name,args) \	102	#define NEED_SUCCESS(name,args) \
39	do { \	103	do { \
40	cl_int res = name args; \	104	res = cl ## name args; \
41	\	105	\
42	if (res) \	106	if (res) \
43	FAIL (name, res); \	107	FAIL (name); \
44	} while (0)	108	} while (0)
45		109
		110	#define NEED_SUCCESS_ARG(retdecl, name, args) \
		111	retdecl = cl ## name args; \
		112	if (res) \
		113	FAIL (name);
		114
		115	/*****************************************************************************/
		116
		117	#define NEW_MORTAL_OBJ(class,ptr) sv_setref_pv (sv_newmortal (), class, ptr)
		118	#define XPUSH_NEW_OBJ(class,ptr) XPUSHs (NEW_MORTAL_OBJ (class, ptr))
		119
		120	static void *
		121	SvPTROBJ (const char *func, const char *svname, SV *sv, const char *pkg)
		122	{
		123	if (SvROK (sv) && sv_derived_from (sv, pkg))
		124	return (void *)SvIV (SvRV (sv));
		125
		126	croak ("%s: %s is not of type %s", func, svname, pkg);
		127	}
		128
		129	/*****************************************************************************/
		130
		131	static size_t
		132	img_row_pitch (cl_mem img)
		133	{
		134	size_t res;
		135	clGetImageInfo (img, CL_IMAGE_ROW_PITCH, sizeof (res), &res, 0);
		136	return res;
		137	}
		138
		139	static cl_event *
		140	event_list (SV **items, int count)
		141	{
		142	cl_event *list = tmpbuf (sizeof (cl_event) * count);
		143
		144	while (count--)
		145	list [count] = SvPTROBJ ("clEnqueue", "wait_events", items [count], "OpenCL::Event");
		146
		147	return list;
		148	}
		149
		150	#define EVENT_LIST(items,count) \
		151	cl_uint event_list_count = (count); \
		152	cl_event *event_list_ptr = event_list (&ST (items), event_list_count)
		153
		154	#define INFO(class) \
		155	{ \
		156	size_t size; \
		157	NEED_SUCCESS (Get ## class ## Info, (this, name, 0, 0, &size)); \
		158	SV *sv = sv_2mortal (newSV (size)); \
		159	SvUPGRADE (sv, SVt_PV); \
		160	SvPOK_only (sv); \
		161	SvCUR_set (sv, size); \
		162	NEED_SUCCESS (Get ## class ## Info, (this, name, size, SvPVX (sv), 0)); \
		163	XPUSHs (sv); \
		164	}
		165
46	MODULE = OpenCL PACKAGE = OpenCL	166	MODULE = OpenCL PACKAGE = OpenCL
		167
		168	PROTOTYPES: ENABLE
47		169
48	BOOT:	170	BOOT:
49	{	171	{
50	HV *stash = gv_stashpv ("OpenCL", 1);	172	HV *stash = gv_stashpv ("OpenCL", 1);
51	static const struct {
52	const char *name;
53	IV iv;
54	} *civ, const_iv[] = {	173	static const ivstr *civ, const_iv[] = {
55	#define const_iv(name) { # name, (IV)CL_ ## name },	174	{ sizeof (cl_char ), "SIZEOF_CHAR" },
		175	{ sizeof (cl_uchar ), "SIZEOF_UCHAR" },
		176	{ sizeof (cl_short ), "SIZEOF_SHORT" },
		177	{ sizeof (cl_ushort), "SIZEOF_USHORT" },
		178	{ sizeof (cl_int ), "SIZEOF_INT" },
		179	{ sizeof (cl_uint ), "SIZEOF_UINT" },
		180	{ sizeof (cl_long ), "SIZEOF_LONG" },
		181	{ sizeof (cl_ulong ), "SIZEOF_ULONG" },
		182	{ sizeof (cl_half ), "SIZEOF_HALF" },
		183	{ sizeof (cl_float ), "SIZEOF_FLOAT" },
		184	{ sizeof (cl_double), "SIZEOF_DOUBLE" },
56	#include "constiv.h"	185	#include "constiv.h"
57	};	186	};
58	for (civ = const_iv + sizeof (const_iv) / sizeof (const_iv [0]); civ > const_iv; civ--)	187	for (civ = const_iv + sizeof (const_iv) / sizeof (const_iv [0]); civ > const_iv; civ--)
59	newCONSTSUB (stash, (char *)civ[-1].name, newSViv (civ[-1].iv));	188	newCONSTSUB (stash, (char *)civ[-1].name, newSViv (civ[-1].iv));
60	}	189	}
61		190
		191	cl_int
		192	errno ()
		193	CODE:
		194	errno = res;
		195
		196	const char *
		197	err2str (cl_int err)
		198
		199	const char *
		200	enum2str (cl_uint value)
		201
62	void	202	void
63	platforms ()	203	platforms ()
64	PPCODE:	204	PPCODE:
65	{
66	cl_platform_id *list;	205	cl_platform_id *list;
67	cl_uint count;	206	cl_uint count;
68	int i;	207	int i;
69		208
70	NEED_SUCCESS (clGetPlatformIDs, (0, 0, &count));	209	NEED_SUCCESS (GetPlatformIDs, (0, 0, &count));
71	Newx (list, count, cl_platform_id);	210	list = tmpbuf (sizeof (*list) * count);
72	NEED_SUCCESS (clGetPlatformIDs, (count, list, 0));	211	NEED_SUCCESS (GetPlatformIDs, (count, list, 0));
73		212
74	EXTEND (SP, count);	213	EXTEND (SP, count);
75	for (i = 0; i < count; ++i)	214	for (i = 0; i < count; ++i)
		215	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Platform", list [i]));
		216
		217	void
		218	context_from_type (FUTURE properties = 0, cl_device_type type = CL_DEVICE_TYPE_DEFAULT, FUTURE notify = 0)
		219	PPCODE:
		220	NEED_SUCCESS_ARG (cl_context ctx, CreateContextFromType, (0, type, 0, 0, &res));
		221	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);
		222
		223	void
		224	context (FUTURE properties, FUTURE devices, FUTURE notify = 0)
		225	PPCODE:
		226	/* der Gipfel der Kunst */
		227
		228	void
		229	wait_for_events (...)
		230	CODE:
		231	EVENT_LIST (0, items);
		232	NEED_SUCCESS (WaitForEvents, (event_list_count, event_list_ptr));
		233
		234	PROTOTYPES: DISABLE
		235
		236	MODULE = OpenCL PACKAGE = OpenCL::Platform
		237
		238	void
		239	info (OpenCL::Platform this, cl_platform_info name)
		240	PPCODE:
		241	INFO (Platform)
		242
		243	#BEGIN:platform
		244
		245	void
		246	profile (OpenCL::Platform this)
		247	PPCODE:
		248	size_t size;
		249	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_PROFILE, 0, 0, &size));
		250	char *value = tmpbuf (size);
		251	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_PROFILE, size, value, 0));
		252	int i, n = 1;
		253	EXTEND (SP, n);
		254	for (i = 0; i < n; ++i)
		255	PUSHs (sv_2mortal (newSVpv (value, 0)));
		256
		257	void
		258	version (OpenCL::Platform this)
		259	PPCODE:
		260	size_t size;
		261	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_VERSION, 0, 0, &size));
		262	char *value = tmpbuf (size);
		263	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_VERSION, size, value, 0));
		264	int i, n = 1;
		265	EXTEND (SP, n);
		266	for (i = 0; i < n; ++i)
		267	PUSHs (sv_2mortal (newSVpv (value, 0)));
		268
		269	void
		270	name (OpenCL::Platform this)
		271	PPCODE:
		272	size_t size;
		273	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_NAME, 0, 0, &size));
		274	char *value = tmpbuf (size);
		275	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_NAME, size, value, 0));
		276	int i, n = 1;
		277	EXTEND (SP, n);
		278	for (i = 0; i < n; ++i)
		279	PUSHs (sv_2mortal (newSVpv (value, 0)));
		280
		281	void
		282	vendor (OpenCL::Platform this)
		283	PPCODE:
		284	size_t size;
		285	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_VENDOR, 0, 0, &size));
		286	char *value = tmpbuf (size);
		287	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_VENDOR, size, value, 0));
		288	int i, n = 1;
		289	EXTEND (SP, n);
		290	for (i = 0; i < n; ++i)
		291	PUSHs (sv_2mortal (newSVpv (value, 0)));
		292
		293	void
		294	extensions (OpenCL::Platform this)
		295	PPCODE:
		296	size_t size;
		297	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_EXTENSIONS, 0, 0, &size));
		298	char *value = tmpbuf (size);
		299	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_EXTENSIONS, size, value, 0));
		300	int i, n = 1;
		301	EXTEND (SP, n);
		302	for (i = 0; i < n; ++i)
		303	PUSHs (sv_2mortal (newSVpv (value, 0)));
		304
		305	#END:platform
		306
		307	void
		308	devices (OpenCL::Platform this, cl_device_type type = CL_DEVICE_TYPE_ALL)
		309	PPCODE:
		310	cl_device_id *list;
		311	cl_uint count;
		312	int i;
		313
		314	NEED_SUCCESS (GetDeviceIDs, (this, type, 0, 0, &count));
		315	list = tmpbuf (sizeof (*list) * count);
		316	NEED_SUCCESS (GetDeviceIDs, (this, type, count, list, 0));
		317
		318	EXTEND (SP, count);
		319	for (i = 0; i < count; ++i)
76	PUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Platform", list [i]));	320	PUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Device", list [i]));
77		321
78	Safefree (list);	322	void
		323	context (OpenCL::Platform this, FUTURE properties, SV *devices, FUTURE notify = 0)
		324	PPCODE:
		325	if (!SvROK (devices) || SvTYPE (SvRV (devices)) != SVt_PVAV)
		326	croak ("OpenCL::Platform argument 'device' must be an arrayref with device objects, in call");
		327
		328	AV *av = (AV *)SvRV (devices);
		329	cl_uint num_devices = av_len (av) + 1;
		330	cl_device_id *device_list = tmpbuf (sizeof (cl_device_id) * num_devices);
		331	int i;
		332
		333	for (i = num_devices; i--; )
		334	device_list [i] = SvPTROBJ ("clCreateContext", "devices", *av_fetch (av, i, 0), "OpenCL::Device");
		335
		336	NEED_SUCCESS_ARG (cl_context ctx, CreateContext, (0, num_devices, device_list, 0, 0, &res));
		337	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);
		338
		339	void
		340	context_from_type (OpenCL::Platform this, FUTURE properties = 0, cl_device_type type = CL_DEVICE_TYPE_DEFAULT, FUTURE notify = 0)
		341	PPCODE:
		342	cl_context_properties props[] = { CL_CONTEXT_PLATFORM, (cl_context_properties)this, 0 };
		343	NEED_SUCCESS_ARG (cl_context ctx, CreateContextFromType, (props, type, 0, 0, &res));
		344	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);
		345
		346	MODULE = OpenCL PACKAGE = OpenCL::Device
		347
		348	void
		349	info (OpenCL::Device this, cl_device_info name)
		350	PPCODE:
		351	INFO (Device)
		352
		353	#BEGIN:device
		354
		355	void
		356	type (OpenCL::Device this)
		357	PPCODE:
		358	cl_device_type value [1];
		359	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_TYPE, sizeof (value), value, 0));
		360	EXTEND (SP, 1);
		361	const int i = 0;
		362	PUSHs (sv_2mortal (newSViv (value [i])));
		363
		364	void
		365	vendor_id (OpenCL::Device this)
		366	PPCODE:
		367	cl_uint value [1];
		368	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VENDOR_ID, sizeof (value), value, 0));
		369	EXTEND (SP, 1);
		370	const int i = 0;
		371	PUSHs (sv_2mortal (newSVuv (value [i])));
		372
		373	void
		374	max_compute_units (OpenCL::Device this)
		375	PPCODE:
		376	cl_uint value [1];
		377	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_COMPUTE_UNITS, sizeof (value), value, 0));
		378	EXTEND (SP, 1);
		379	const int i = 0;
		380	PUSHs (sv_2mortal (newSVuv (value [i])));
		381
		382	void
		383	max_work_item_dimensions (OpenCL::Device this)
		384	PPCODE:
		385	cl_uint value [1];
		386	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS, sizeof (value), value, 0));
		387	EXTEND (SP, 1);
		388	const int i = 0;
		389	PUSHs (sv_2mortal (newSVuv (value [i])));
		390
		391	void
		392	max_work_group_size (OpenCL::Device this)
		393	PPCODE:
		394	size_t value [1];
		395	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WORK_GROUP_SIZE, sizeof (value), value, 0));
		396	EXTEND (SP, 1);
		397	const int i = 0;
		398	PUSHs (sv_2mortal (newSVuv (value [i])));
		399
		400	void
		401	max_work_item_sizes (OpenCL::Device this)
		402	PPCODE:
		403	size_t size;
		404	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WORK_ITEM_SIZES, 0, 0, &size));
		405	size_t *value = tmpbuf (size);
		406	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WORK_ITEM_SIZES, size, value, 0));
		407	int i, n = size / sizeof (*value);
		408	EXTEND (SP, n);
		409	for (i = 0; i < n; ++i)
		410	PUSHs (sv_2mortal (newSVuv (value [i])));
		411
		412	void
		413	preferred_vector_width_char (OpenCL::Device this)
		414	PPCODE:
		415	cl_uint value [1];
		416	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR, sizeof (value), value, 0));
		417	EXTEND (SP, 1);
		418	const int i = 0;
		419	PUSHs (sv_2mortal (newSVuv (value [i])));
		420
		421	void
		422	preferred_vector_width_short (OpenCL::Device this)
		423	PPCODE:
		424	cl_uint value [1];
		425	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT, sizeof (value), value, 0));
		426	EXTEND (SP, 1);
		427	const int i = 0;
		428	PUSHs (sv_2mortal (newSVuv (value [i])));
		429
		430	void
		431	preferred_vector_width_int (OpenCL::Device this)
		432	PPCODE:
		433	cl_uint value [1];
		434	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT, sizeof (value), value, 0));
		435	EXTEND (SP, 1);
		436	const int i = 0;
		437	PUSHs (sv_2mortal (newSVuv (value [i])));
		438
		439	void
		440	preferred_vector_width_long (OpenCL::Device this)
		441	PPCODE:
		442	cl_uint value [1];
		443	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG, sizeof (value), value, 0));
		444	EXTEND (SP, 1);
		445	const int i = 0;
		446	PUSHs (sv_2mortal (newSVuv (value [i])));
		447
		448	void
		449	preferred_vector_width_float (OpenCL::Device this)
		450	PPCODE:
		451	cl_uint value [1];
		452	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT, sizeof (value), value, 0));
		453	EXTEND (SP, 1);
		454	const int i = 0;
		455	PUSHs (sv_2mortal (newSVuv (value [i])));
		456
		457	void
		458	preferred_vector_width_double (OpenCL::Device this)
		459	PPCODE:
		460	cl_uint value [1];
		461	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE, sizeof (value), value, 0));
		462	EXTEND (SP, 1);
		463	const int i = 0;
		464	PUSHs (sv_2mortal (newSVuv (value [i])));
		465
		466	void
		467	max_clock_frequency (OpenCL::Device this)
		468	PPCODE:
		469	cl_uint value [1];
		470	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_CLOCK_FREQUENCY, sizeof (value), value, 0));
		471	EXTEND (SP, 1);
		472	const int i = 0;
		473	PUSHs (sv_2mortal (newSVuv (value [i])));
		474
		475	void
		476	address_bits (OpenCL::Device this)
		477	PPCODE:
		478	cl_bitfield value [1];
		479	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_ADDRESS_BITS, sizeof (value), value, 0));
		480	EXTEND (SP, 1);
		481	const int i = 0;
		482	PUSHs (sv_2mortal (newSVuv (value [i])));
		483
		484	void
		485	max_read_image_args (OpenCL::Device this)
		486	PPCODE:
		487	cl_uint value [1];
		488	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_READ_IMAGE_ARGS, sizeof (value), value, 0));
		489	EXTEND (SP, 1);
		490	const int i = 0;
		491	PUSHs (sv_2mortal (newSVuv (value [i])));
		492
		493	void
		494	max_write_image_args (OpenCL::Device this)
		495	PPCODE:
		496	cl_uint value [1];
		497	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WRITE_IMAGE_ARGS, sizeof (value), value, 0));
		498	EXTEND (SP, 1);
		499	const int i = 0;
		500	PUSHs (sv_2mortal (newSVuv (value [i])));
		501
		502	void
		503	max_mem_alloc_size (OpenCL::Device this)
		504	PPCODE:
		505	cl_ulong value [1];
		506	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_MEM_ALLOC_SIZE, sizeof (value), value, 0));
		507	EXTEND (SP, 1);
		508	const int i = 0;
		509	PUSHs (sv_2mortal (newSVuv (value [i])));
		510
		511	void
		512	image2d_max_width (OpenCL::Device this)
		513	PPCODE:
		514	size_t value [1];
		515	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE2D_MAX_WIDTH, sizeof (value), value, 0));
		516	EXTEND (SP, 1);
		517	const int i = 0;
		518	PUSHs (sv_2mortal (newSVuv (value [i])));
		519
		520	void
		521	image2d_max_height (OpenCL::Device this)
		522	PPCODE:
		523	size_t value [1];
		524	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE2D_MAX_HEIGHT, sizeof (value), value, 0));
		525	EXTEND (SP, 1);
		526	const int i = 0;
		527	PUSHs (sv_2mortal (newSVuv (value [i])));
		528
		529	void
		530	image3d_max_width (OpenCL::Device this)
		531	PPCODE:
		532	size_t value [1];
		533	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE3D_MAX_WIDTH, sizeof (value), value, 0));
		534	EXTEND (SP, 1);
		535	const int i = 0;
		536	PUSHs (sv_2mortal (newSVuv (value [i])));
		537
		538	void
		539	image3d_max_height (OpenCL::Device this)
		540	PPCODE:
		541	size_t value [1];
		542	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE3D_MAX_HEIGHT, sizeof (value), value, 0));
		543	EXTEND (SP, 1);
		544	const int i = 0;
		545	PUSHs (sv_2mortal (newSVuv (value [i])));
		546
		547	void
		548	image3d_max_depth (OpenCL::Device this)
		549	PPCODE:
		550	size_t value [1];
		551	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE3D_MAX_DEPTH, sizeof (value), value, 0));
		552	EXTEND (SP, 1);
		553	const int i = 0;
		554	PUSHs (sv_2mortal (newSVuv (value [i])));
		555
		556	void
		557	image_support (OpenCL::Device this)
		558	PPCODE:
		559	cl_uint value [1];
		560	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE_SUPPORT, sizeof (value), value, 0));
		561	EXTEND (SP, 1);
		562	const int i = 0;
		563	PUSHs (sv_2mortal (newSVuv (value [i])));
		564
		565	void
		566	max_parameter_size (OpenCL::Device this)
		567	PPCODE:
		568	size_t value [1];
		569	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_PARAMETER_SIZE, sizeof (value), value, 0));
		570	EXTEND (SP, 1);
		571	const int i = 0;
		572	PUSHs (sv_2mortal (newSVuv (value [i])));
		573
		574	void
		575	max_samplers (OpenCL::Device this)
		576	PPCODE:
		577	cl_uint value [1];
		578	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_SAMPLERS, sizeof (value), value, 0));
		579	EXTEND (SP, 1);
		580	const int i = 0;
		581	PUSHs (sv_2mortal (newSVuv (value [i])));
		582
		583	void
		584	mem_base_addr_align (OpenCL::Device this)
		585	PPCODE:
		586	cl_uint value [1];
		587	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MEM_BASE_ADDR_ALIGN, sizeof (value), value, 0));
		588	EXTEND (SP, 1);
		589	const int i = 0;
		590	PUSHs (sv_2mortal (newSVuv (value [i])));
		591
		592	void
		593	min_data_type_align_size (OpenCL::Device this)
		594	PPCODE:
		595	cl_uint value [1];
		596	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE, sizeof (value), value, 0));
		597	EXTEND (SP, 1);
		598	const int i = 0;
		599	PUSHs (sv_2mortal (newSVuv (value [i])));
		600
		601	void
		602	single_fp_config (OpenCL::Device this)
		603	PPCODE:
		604	cl_device_fp_config value [1];
		605	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_SINGLE_FP_CONFIG, sizeof (value), value, 0));
		606	EXTEND (SP, 1);
		607	const int i = 0;
		608	PUSHs (sv_2mortal (newSVuv (value [i])));
		609
		610	void
		611	global_mem_cache_type (OpenCL::Device this)
		612	PPCODE:
		613	cl_device_mem_cache_type value [1];
		614	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_GLOBAL_MEM_CACHE_TYPE, sizeof (value), value, 0));
		615	EXTEND (SP, 1);
		616	const int i = 0;
		617	PUSHs (sv_2mortal (newSVuv (value [i])));
		618
		619	void
		620	global_mem_cacheline_size (OpenCL::Device this)
		621	PPCODE:
		622	cl_uint value [1];
		623	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE, sizeof (value), value, 0));
		624	EXTEND (SP, 1);
		625	const int i = 0;
		626	PUSHs (sv_2mortal (newSVuv (value [i])));
		627
		628	void
		629	global_mem_cache_size (OpenCL::Device this)
		630	PPCODE:
		631	cl_ulong value [1];
		632	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_GLOBAL_MEM_CACHE_SIZE, sizeof (value), value, 0));
		633	EXTEND (SP, 1);
		634	const int i = 0;
		635	PUSHs (sv_2mortal (newSVuv (value [i])));
		636
		637	void
		638	global_mem_size (OpenCL::Device this)
		639	PPCODE:
		640	cl_ulong value [1];
		641	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_GLOBAL_MEM_SIZE, sizeof (value), value, 0));
		642	EXTEND (SP, 1);
		643	const int i = 0;
		644	PUSHs (sv_2mortal (newSVuv (value [i])));
		645
		646	void
		647	max_constant_buffer_size (OpenCL::Device this)
		648	PPCODE:
		649	cl_ulong value [1];
		650	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE, sizeof (value), value, 0));
		651	EXTEND (SP, 1);
		652	const int i = 0;
		653	PUSHs (sv_2mortal (newSVuv (value [i])));
		654
		655	void
		656	max_constant_args (OpenCL::Device this)
		657	PPCODE:
		658	cl_uint value [1];
		659	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_CONSTANT_ARGS, sizeof (value), value, 0));
		660	EXTEND (SP, 1);
		661	const int i = 0;
		662	PUSHs (sv_2mortal (newSVuv (value [i])));
		663
		664	void
		665	local_mem_type (OpenCL::Device this)
		666	PPCODE:
		667	cl_device_local_mem_type value [1];
		668	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_LOCAL_MEM_TYPE, sizeof (value), value, 0));
		669	EXTEND (SP, 1);
		670	const int i = 0;
		671	PUSHs (sv_2mortal (newSVuv (value [i])));
		672
		673	void
		674	local_mem_size (OpenCL::Device this)
		675	PPCODE:
		676	cl_ulong value [1];
		677	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_LOCAL_MEM_SIZE, sizeof (value), value, 0));
		678	EXTEND (SP, 1);
		679	const int i = 0;
		680	PUSHs (sv_2mortal (newSVuv (value [i])));
		681
		682	void
		683	error_correction_support (OpenCL::Device this)
		684	PPCODE:
		685	cl_bool value [1];
		686	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_ERROR_CORRECTION_SUPPORT, sizeof (value), value, 0));
		687	EXTEND (SP, 1);
		688	const int i = 0;
		689	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		690
		691	void
		692	profiling_timer_resolution (OpenCL::Device this)
		693	PPCODE:
		694	size_t value [1];
		695	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PROFILING_TIMER_RESOLUTION, sizeof (value), value, 0));
		696	EXTEND (SP, 1);
		697	const int i = 0;
		698	PUSHs (sv_2mortal (newSVuv (value [i])));
		699
		700	void
		701	endian_little (OpenCL::Device this)
		702	PPCODE:
		703	cl_bool value [1];
		704	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_ENDIAN_LITTLE, sizeof (value), value, 0));
		705	EXTEND (SP, 1);
		706	const int i = 0;
		707	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		708
		709	void
		710	available (OpenCL::Device this)
		711	PPCODE:
		712	cl_bool value [1];
		713	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_AVAILABLE, sizeof (value), value, 0));
		714	EXTEND (SP, 1);
		715	const int i = 0;
		716	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		717
		718	void
		719	compiler_available (OpenCL::Device this)
		720	PPCODE:
		721	cl_bool value [1];
		722	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_COMPILER_AVAILABLE, sizeof (value), value, 0));
		723	EXTEND (SP, 1);
		724	const int i = 0;
		725	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		726
		727	void
		728	execution_capabilities (OpenCL::Device this)
		729	PPCODE:
		730	cl_device_exec_capabilities value [1];
		731	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_EXECUTION_CAPABILITIES, sizeof (value), value, 0));
		732	EXTEND (SP, 1);
		733	const int i = 0;
		734	PUSHs (sv_2mortal (newSVuv (value [i])));
		735
		736	void
		737	properties (OpenCL::Device this)
		738	PPCODE:
		739	cl_command_queue_properties value [1];
		740	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_QUEUE_PROPERTIES, sizeof (value), value, 0));
		741	EXTEND (SP, 1);
		742	const int i = 0;
		743	PUSHs (sv_2mortal (newSViv (value [i])));
		744
		745	void
		746	platform (OpenCL::Device this)
		747	PPCODE:
		748	cl_platform_id value [1];
		749	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PLATFORM, sizeof (value), value, 0));
		750	EXTEND (SP, 1);
		751	const int i = 0;
		752	{
		753	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Platform", value [i]));
		754	}
		755
		756	void
		757	name (OpenCL::Device this)
		758	PPCODE:
		759	size_t size;
		760	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NAME, 0, 0, &size));
		761	char *value = tmpbuf (size);
		762	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NAME, size, value, 0));
		763	int i, n = 1;
		764	EXTEND (SP, n);
		765	for (i = 0; i < n; ++i)
		766	PUSHs (sv_2mortal (newSVpv (value, 0)));
		767
		768	void
		769	vendor (OpenCL::Device this)
		770	PPCODE:
		771	size_t size;
		772	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VENDOR, 0, 0, &size));
		773	char *value = tmpbuf (size);
		774	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VENDOR, size, value, 0));
		775	int i, n = 1;
		776	EXTEND (SP, n);
		777	for (i = 0; i < n; ++i)
		778	PUSHs (sv_2mortal (newSVpv (value, 0)));
		779
		780	void
		781	driver_version (OpenCL::Device this)
		782	PPCODE:
		783	size_t size;
		784	NEED_SUCCESS (GetDeviceInfo, (this, CL_DRIVER_VERSION, 0, 0, &size));
		785	char *value = tmpbuf (size);
		786	NEED_SUCCESS (GetDeviceInfo, (this, CL_DRIVER_VERSION, size, value, 0));
		787	int i, n = 1;
		788	EXTEND (SP, n);
		789	for (i = 0; i < n; ++i)
		790	PUSHs (sv_2mortal (newSVpv (value, 0)));
		791
		792	void
		793	profile (OpenCL::Device this)
		794	PPCODE:
		795	size_t size;
		796	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PROFILE, 0, 0, &size));
		797	char *value = tmpbuf (size);
		798	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PROFILE, size, value, 0));
		799	int i, n = 1;
		800	EXTEND (SP, n);
		801	for (i = 0; i < n; ++i)
		802	PUSHs (sv_2mortal (newSVpv (value, 0)));
		803
		804	void
		805	version (OpenCL::Device this)
		806	PPCODE:
		807	size_t size;
		808	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VERSION, 0, 0, &size));
		809	char *value = tmpbuf (size);
		810	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VERSION, size, value, 0));
		811	int i, n = 1;
		812	EXTEND (SP, n);
		813	for (i = 0; i < n; ++i)
		814	PUSHs (sv_2mortal (newSVpv (value, 0)));
		815
		816	void
		817	extensions (OpenCL::Device this)
		818	PPCODE:
		819	size_t size;
		820	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_EXTENSIONS, 0, 0, &size));
		821	char *value = tmpbuf (size);
		822	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_EXTENSIONS, size, value, 0));
		823	int i, n = 1;
		824	EXTEND (SP, n);
		825	for (i = 0; i < n; ++i)
		826	PUSHs (sv_2mortal (newSVpv (value, 0)));
		827
		828	void
		829	preferred_vector_width_half (OpenCL::Device this)
		830	PPCODE:
		831	cl_uint value [1];
		832	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF, sizeof (value), value, 0));
		833	EXTEND (SP, 1);
		834	const int i = 0;
		835	PUSHs (sv_2mortal (newSVuv (value [i])));
		836
		837	void
		838	native_vector_width_char (OpenCL::Device this)
		839	PPCODE:
		840	cl_uint value [1];
		841	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR, sizeof (value), value, 0));
		842	EXTEND (SP, 1);
		843	const int i = 0;
		844	PUSHs (sv_2mortal (newSVuv (value [i])));
		845
		846	void
		847	native_vector_width_short (OpenCL::Device this)
		848	PPCODE:
		849	cl_uint value [1];
		850	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT, sizeof (value), value, 0));
		851	EXTEND (SP, 1);
		852	const int i = 0;
		853	PUSHs (sv_2mortal (newSVuv (value [i])));
		854
		855	void
		856	native_vector_width_int (OpenCL::Device this)
		857	PPCODE:
		858	cl_uint value [1];
		859	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_INT, sizeof (value), value, 0));
		860	EXTEND (SP, 1);
		861	const int i = 0;
		862	PUSHs (sv_2mortal (newSVuv (value [i])));
		863
		864	void
		865	native_vector_width_long (OpenCL::Device this)
		866	PPCODE:
		867	cl_uint value [1];
		868	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG, sizeof (value), value, 0));
		869	EXTEND (SP, 1);
		870	const int i = 0;
		871	PUSHs (sv_2mortal (newSVuv (value [i])));
		872
		873	void
		874	native_vector_width_float (OpenCL::Device this)
		875	PPCODE:
		876	cl_uint value [1];
		877	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT, sizeof (value), value, 0));
		878	EXTEND (SP, 1);
		879	const int i = 0;
		880	PUSHs (sv_2mortal (newSVuv (value [i])));
		881
		882	void
		883	native_vector_width_double (OpenCL::Device this)
		884	PPCODE:
		885	cl_uint value [1];
		886	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE, sizeof (value), value, 0));
		887	EXTEND (SP, 1);
		888	const int i = 0;
		889	PUSHs (sv_2mortal (newSVuv (value [i])));
		890
		891	void
		892	native_vector_width_half (OpenCL::Device this)
		893	PPCODE:
		894	cl_uint value [1];
		895	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF, sizeof (value), value, 0));
		896	EXTEND (SP, 1);
		897	const int i = 0;
		898	PUSHs (sv_2mortal (newSVuv (value [i])));
		899
		900	void
		901	double_fp_config (OpenCL::Device this)
		902	PPCODE:
		903	cl_device_fp_config value [1];
		904	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_DOUBLE_FP_CONFIG, sizeof (value), value, 0));
		905	EXTEND (SP, 1);
		906	const int i = 0;
		907	PUSHs (sv_2mortal (newSVuv (value [i])));
		908
		909	void
		910	half_fp_config (OpenCL::Device this)
		911	PPCODE:
		912	cl_device_fp_config value [1];
		913	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_HALF_FP_CONFIG, sizeof (value), value, 0));
		914	EXTEND (SP, 1);
		915	const int i = 0;
		916	PUSHs (sv_2mortal (newSVuv (value [i])));
		917
		918	void
		919	host_unified_memory (OpenCL::Device this)
		920	PPCODE:
		921	cl_bool value [1];
		922	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_HOST_UNIFIED_MEMORY, sizeof (value), value, 0));
		923	EXTEND (SP, 1);
		924	const int i = 0;
		925	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		926
		927	void
		928	parent_device_ext (OpenCL::Device this)
		929	PPCODE:
		930	cl_device_id value [1];
		931	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARENT_DEVICE_EXT, sizeof (value), value, 0));
		932	EXTEND (SP, 1);
		933	const int i = 0;
		934	{
		935	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Device", value [i]));
		936	}
		937
		938	void
		939	partition_types_ext (OpenCL::Device this)
		940	PPCODE:
		941	size_t size;
		942	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARTITION_TYPES_EXT, 0, 0, &size));
		943	cl_device_partition_property_ext *value = tmpbuf (size);
		944	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARTITION_TYPES_EXT, size, value, 0));
		945	int i, n = size / sizeof (*value);
		946	EXTEND (SP, n);
		947	for (i = 0; i < n; ++i)
		948	PUSHs (sv_2mortal (newSVuv (value [i])));
		949
		950	void
		951	affinity_domains_ext (OpenCL::Device this)
		952	PPCODE:
		953	size_t size;
		954	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_AFFINITY_DOMAINS_EXT, 0, 0, &size));
		955	cl_device_partition_property_ext *value = tmpbuf (size);
		956	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_AFFINITY_DOMAINS_EXT, size, value, 0));
		957	int i, n = size / sizeof (*value);
		958	EXTEND (SP, n);
		959	for (i = 0; i < n; ++i)
		960	PUSHs (sv_2mortal (newSVuv (value [i])));
		961
		962	void
		963	reference_count_ext (OpenCL::Device this)
		964	PPCODE:
		965	cl_uint value [1];
		966	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_REFERENCE_COUNT_EXT , sizeof (value), value, 0));
		967	EXTEND (SP, 1);
		968	const int i = 0;
		969	PUSHs (sv_2mortal (newSVuv (value [i])));
		970
		971	void
		972	partition_style_ext (OpenCL::Device this)
		973	PPCODE:
		974	size_t size;
		975	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARTITION_STYLE_EXT, 0, 0, &size));
		976	cl_device_partition_property_ext *value = tmpbuf (size);
		977	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARTITION_STYLE_EXT, size, value, 0));
		978	int i, n = size / sizeof (*value);
		979	EXTEND (SP, n);
		980	for (i = 0; i < n; ++i)
		981	PUSHs (sv_2mortal (newSVuv (value [i])));
		982
		983	#END:device
		984
		985	MODULE = OpenCL PACKAGE = OpenCL::Context
		986
		987	void
		988	DESTROY (OpenCL::Context context)
		989	CODE:
		990	clReleaseContext (context);
		991
		992	void
		993	info (OpenCL::Context this, cl_context_info name)
		994	PPCODE:
		995	INFO (Context)
		996
		997	void
		998	queue (OpenCL::Context this, OpenCL::Device device, cl_command_queue_properties properties = 0)
		999	PPCODE:
		1000	NEED_SUCCESS_ARG (cl_command_queue queue, CreateCommandQueue, (this, device, properties, &res));
		1001	XPUSH_NEW_OBJ ("OpenCL::Queue", queue);
		1002
		1003	void
		1004	user_event (OpenCL::Context this)
		1005	PPCODE:
		1006	NEED_SUCCESS_ARG (cl_event ev, CreateUserEvent, (this, &res));
		1007	XPUSH_NEW_OBJ ("OpenCL::UserEvent", ev);
		1008
		1009	void
		1010	buffer (OpenCL::Context this, cl_mem_flags flags, size_t len)
		1011	PPCODE:
		1012	if (flags & (CL_MEM_USE_HOST_PTR | CL_MEM_COPY_HOST_PTR))
		1013	croak ("clCreateBuffer: cannot use/copy host ptr when no data is given, use $context->buffer_sv instead?");
		1014
		1015	NEED_SUCCESS_ARG (cl_mem mem, CreateBuffer, (this, flags, len, 0, &res));
		1016	XPUSH_NEW_OBJ ("OpenCL::Buffer", mem);
		1017
		1018	void
		1019	buffer_sv (OpenCL::Context this, cl_mem_flags flags, SV *data)
		1020	PPCODE:
		1021	STRLEN len;
		1022	char *ptr = SvPVbyte (data, len);
		1023
		1024	if (!(flags & (CL_MEM_USE_HOST_PTR | CL_MEM_COPY_HOST_PTR)))
		1025	croak ("clCreateBuffer: have to specify use or copy host ptr when buffer data is given, use $context->buffer instead?");
		1026
		1027	NEED_SUCCESS_ARG (cl_mem mem, CreateBuffer, (this, flags, len, ptr, &res));
		1028	XPUSH_NEW_OBJ ("OpenCL::Buffer", mem);
		1029
		1030	void
		1031	image2d (OpenCL::Context this, cl_mem_flags flags, cl_channel_order channel_order, cl_channel_type channel_type, size_t width, size_t height, size_t row_pitch = 0, SV *data = &PL_sv_undef)
		1032	PPCODE:
		1033	STRLEN len;
		1034	char *ptr = SvPVbyte (data, len);
		1035	const cl_image_format format = { channel_order, channel_type };
		1036	NEED_SUCCESS_ARG (cl_mem mem, CreateImage2D, (this, flags, &format, width, height, row_pitch, ptr, &res));
		1037	XPUSH_NEW_OBJ ("OpenCL::Image2D", mem);
		1038
		1039	void
		1040	image3d (OpenCL::Context this, cl_mem_flags flags, cl_channel_order channel_order, cl_channel_type channel_type, size_t width, size_t height, size_t depth, size_t row_pitch = 0, size_t slice_pitch = 0, SV *data = &PL_sv_undef)
		1041	PPCODE:
		1042	STRLEN len;
		1043	char *ptr = SvPVbyte (data, len);
		1044	const cl_image_format format = { channel_order, channel_type };
		1045	NEED_SUCCESS_ARG (cl_mem mem, CreateImage3D, (this, flags, &format, width, height, depth, row_pitch, slice_pitch, ptr, &res));
		1046	XPUSH_NEW_OBJ ("OpenCL::Image3D", mem);
		1047
		1048	void
		1049	supported_image_formats (OpenCL::Context this, cl_mem_flags flags, cl_mem_object_type image_type)
		1050	PPCODE:
		1051	{
		1052	cl_uint count;
		1053	cl_image_format *list;
		1054	int i;
		1055
		1056	NEED_SUCCESS (GetSupportedImageFormats, (this, flags, image_type, 0, 0, &count));
		1057	Newx (list, count, cl_image_format);
		1058	NEED_SUCCESS (GetSupportedImageFormats, (this, flags, image_type, count, list, 0));
		1059
		1060	EXTEND (SP, count);
		1061	for (i = 0; i < count; ++i)
		1062	{
		1063	AV *av = newAV ();
		1064	av_store (av, 1, newSVuv (list [i].image_channel_data_type));
		1065	av_store (av, 0, newSVuv (list [i].image_channel_order));
		1066	PUSHs (sv_2mortal (newRV_noinc ((SV *)av)));
		1067	}
79	}	1068	}
80		1069
81	void	1070	void
82	context_from_type_simple (cl_device_type type = CL_DEVICE_TYPE_DEFAULT)	1071	sampler (OpenCL::Context this, cl_bool normalized_coords, cl_addressing_mode addressing_mode, cl_filter_mode filter_mode)
		1072	PPCODE:
		1073	NEED_SUCCESS_ARG (cl_sampler sampler, CreateSampler, (this, normalized_coords, addressing_mode, filter_mode, &res));
		1074	XPUSH_NEW_OBJ ("OpenCL::Sampler", sampler);
		1075
		1076	void
		1077	program_with_source (OpenCL::Context this, SV *program)
		1078	PPCODE:
		1079	STRLEN len;
		1080	size_t len2;
		1081	const char *ptr = SvPVbyte (program, len);
		1082
		1083	len2 = len;
		1084	NEED_SUCCESS_ARG (cl_program prog, CreateProgramWithSource, (this, 1, &ptr, &len2, &res));
		1085	XPUSH_NEW_OBJ ("OpenCL::Program", prog);
		1086
		1087	#BEGIN:context
		1088
		1089	void
		1090	reference_count (OpenCL::Context this)
83	PPCODE:	1091	PPCODE:
84	{	1092	cl_uint value [1];
85	cl_int res;	1093	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_REFERENCE_COUNT, sizeof (value), value, 0));
86	cl_context ctx = clCreateContextFromType (0, type, 0, 0, &res);	1094	EXTEND (SP, 1);
		1095	const int i = 0;
		1096	PUSHs (sv_2mortal (newSVuv (value [i])));
87		1097
		1098	void
		1099	devices (OpenCL::Context this)
		1100	PPCODE:
		1101	size_t size;
		1102	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_DEVICES, 0, 0, &size));
		1103	cl_device_id *value = tmpbuf (size);
		1104	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_DEVICES, size, value, 0));
		1105	int i, n = size / sizeof (*value);
		1106	EXTEND (SP, n);
		1107	for (i = 0; i < n; ++i)
		1108	{
		1109	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Device", value [i]));
		1110	}
		1111
		1112	void
		1113	properties (OpenCL::Context this)
		1114	PPCODE:
		1115	size_t size;
		1116	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_PROPERTIES, 0, 0, &size));
		1117	cl_context_properties *value = tmpbuf (size);
		1118	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_PROPERTIES, size, value, 0));
		1119	int i, n = size / sizeof (*value);
		1120	EXTEND (SP, n);
		1121	for (i = 0; i < n; ++i)
		1122	PUSHs (sv_2mortal (newSVuv ((UV)value [i])));
		1123
		1124	void
		1125	num_devices (OpenCL::Context this)
		1126	PPCODE:
		1127	cl_uint value [1];
		1128	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_NUM_DEVICES, sizeof (value), value, 0));
		1129	EXTEND (SP, 1);
		1130	const int i = 0;
		1131	PUSHs (sv_2mortal (newSVuv (value [i])));
		1132
		1133	#END:context
		1134
		1135	MODULE = OpenCL PACKAGE = OpenCL::Queue
		1136
		1137	void
		1138	DESTROY (OpenCL::Queue this)
		1139	CODE:
		1140	clReleaseCommandQueue (this);
		1141
		1142	void
		1143	enqueue_read_buffer (OpenCL::Queue this, OpenCL::Buffer mem, cl_bool blocking, size_t offset, size_t len, SV *data, ...)
		1144	PPCODE:
		1145	cl_event ev = 0;
		1146	EVENT_LIST (6, items - 6);
		1147
		1148	SvUPGRADE (data, SVt_PV);
		1149	SvGROW (data, len);
		1150	SvPOK_only (data);
		1151	SvCUR_set (data, len);
		1152	NEED_SUCCESS (EnqueueReadBuffer, (this, mem, blocking, offset, len, SvPVX (data), event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1153
88	if (res)	1154	if (ev)
89	FAIL (clCreateContextFromType, res);	1155	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
90		1156
91	XPUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Context", ctx));	1157	void
92	}	1158	enqueue_write_buffer (OpenCL::Queue this, OpenCL::Buffer mem, cl_bool blocking, size_t offset, SV *data, ...)
		1159	PPCODE:
		1160	cl_event ev = 0;
		1161	STRLEN len;
		1162	char *ptr = SvPVbyte (data, len);
		1163	EVENT_LIST (5, items - 5);
93		1164
		1165	NEED_SUCCESS (EnqueueReadBuffer, (this, mem, blocking, offset, len, ptr, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1166
		1167	if (ev)
		1168	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1169
		1170	void
		1171	enqueue_copy_buffer (OpenCL::Queue this, OpenCL::Buffer src, OpenCL::Buffer dst, size_t src_offset, size_t dst_offset, size_t len, ...)
		1172	PPCODE:
		1173	cl_event ev = 0;
		1174	EVENT_LIST (6, items - 6);
		1175
		1176	NEED_SUCCESS (EnqueueCopyBuffer, (this, src, dst, src_offset, dst_offset, len, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1177
		1178	if (ev)
		1179	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1180
		1181	void
		1182	enqueue_read_image (OpenCL::Queue this, OpenCL::Image src, cl_bool blocking, size_t src_x, size_t src_y, size_t src_z, size_t width, size_t height, size_t depth, size_t row_pitch, size_t slice_pitch, SV *data, ...)
		1183	PPCODE:
		1184	cl_event ev = 0;
		1185	const size_t src_origin[3] = { src_x, src_y, src_z };
		1186	const size_t region[3] = { width, height, depth };
		1187	EVENT_LIST (12, items - 12);
		1188
		1189	if (!row_pitch)
		1190	row_pitch = img_row_pitch (src);
		1191
		1192	if (depth > 1 && !slice_pitch)
		1193	slice_pitch = row_pitch * height;
		1194
		1195	size_t len = slice_pitch ? slice_pitch * depth : row_pitch * height;
		1196
		1197	SvUPGRADE (data, SVt_PV);
		1198	SvGROW (data, len);
		1199	SvPOK_only (data);
		1200	SvCUR_set (data, len);
		1201	NEED_SUCCESS (EnqueueReadImage, (this, src, blocking, src_origin, region, row_pitch, slice_pitch, SvPVX (data), event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1202
		1203	if (ev)
		1204	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1205
		1206	void
		1207	enqueue_write_image (OpenCL::Queue this, OpenCL::Image dst, cl_bool blocking, size_t dst_x, size_t dst_y, size_t dst_z, size_t width, size_t height, size_t depth, size_t row_pitch, size_t slice_pitch, SV *data, ...)
		1208	PPCODE:
		1209	cl_event ev = 0;
		1210	const size_t dst_origin[3] = { dst_x, dst_y, dst_z };
		1211	const size_t region[3] = { width, height, depth };
		1212	STRLEN len;
		1213	char *ptr = SvPVbyte (data, len);
		1214	EVENT_LIST (12, items - 12);
		1215
		1216	if (!row_pitch)
		1217	row_pitch = img_row_pitch (dst);
		1218
		1219	if (depth > 1 && !slice_pitch)
		1220	slice_pitch = row_pitch * height;
		1221
		1222	size_t min_len = slice_pitch ? slice_pitch * depth : row_pitch * height;
		1223
		1224	if (len < min_len)
		1225	croak ("clEnqueueWriteImage: data string is shorter than what would be transferred");
		1226
		1227	NEED_SUCCESS (EnqueueWriteImage, (this, dst, blocking, dst_origin, region, row_pitch, slice_pitch, SvPVX (data), event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1228
		1229	if (ev)
		1230	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1231
		1232	void
		1233	enqueue_copy_buffer_rect (OpenCL::Queue this, OpenCL::Buffer src, OpenCL::Buffer dst, size_t src_x, size_t src_y, size_t src_z, size_t dst_x, size_t dst_y, size_t dst_z, size_t width, size_t height, size_t depth, size_t src_row_pitch, size_t src_slice_pitch, size_t dst_row_pitch, size_t dst_slice_pitch, ...)
		1234	PPCODE:
		1235	cl_event ev = 0;
		1236	const size_t src_origin[3] = { src_x, src_y, src_z };
		1237	const size_t dst_origin[3] = { dst_x, dst_y, dst_z };
		1238	const size_t region[3] = { width, height, depth };
		1239	EVENT_LIST (16, items - 16);
		1240
		1241	NEED_SUCCESS (EnqueueCopyBufferRect, (this, src, dst, src_origin, dst_origin, region, src_row_pitch, src_slice_pitch, dst_row_pitch, dst_slice_pitch, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1242
		1243	if (ev)
		1244	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1245
		1246	void
		1247	enqueue_copy_buffer_to_image (OpenCL::Queue this, OpenCL::Buffer src, OpenCL::Image dst, size_t src_offset, size_t dst_x, size_t dst_y, size_t dst_z, size_t width, size_t height, size_t depth, ...)
		1248	PPCODE:
		1249	cl_event ev = 0;
		1250	const size_t dst_origin[3] = { dst_x, dst_y, dst_z };
		1251	const size_t region[3] = { width, height, depth };
		1252	EVENT_LIST (10, items - 10);
		1253
		1254	NEED_SUCCESS (EnqueueCopyBufferToImage, (this, src, dst, src_offset, dst_origin, region, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1255
		1256	if (ev)
		1257	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1258
		1259	void
		1260	enqueue_copy_image (OpenCL::Queue this, OpenCL::Image src, OpenCL::Image dst, size_t src_x, size_t src_y, size_t src_z, size_t dst_x, size_t dst_y, size_t dst_z, size_t width, size_t height, size_t depth, ...)
		1261	PPCODE:
		1262	cl_event ev = 0;
		1263	const size_t src_origin[3] = { src_x, src_y, src_z };
		1264	const size_t dst_origin[3] = { dst_x, dst_y, dst_z };
		1265	const size_t region[3] = { width, height, depth };
		1266	EVENT_LIST (12, items - 12);
		1267
		1268	NEED_SUCCESS (EnqueueCopyImage, (this, src, dst, src_origin, dst_origin, region, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1269
		1270	if (ev)
		1271	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1272
		1273	void
		1274	enqueue_copy_image_to_buffer (OpenCL::Queue this, OpenCL::Image src, OpenCL::Buffer dst, size_t src_x, size_t src_y, size_t src_z, size_t width, size_t height, size_t depth, size_t dst_offset, ...)
		1275	PPCODE:
		1276	cl_event ev = 0;
		1277	const size_t src_origin[3] = { src_x, src_y, src_z };
		1278	const size_t region[3] = { width, height, depth };
		1279	EVENT_LIST (10, items - 10);
		1280
		1281	NEED_SUCCESS (EnqueueCopyImageToBuffer, (this, src, dst, src_origin, region, dst_offset, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1282
		1283	if (ev)
		1284	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1285
		1286	void
		1287	enqueue_task (OpenCL::Queue this, OpenCL::Kernel kernel, ...)
		1288	PPCODE:
		1289	cl_event ev = 0;
		1290	EVENT_LIST (2, items - 2);
		1291
		1292	NEED_SUCCESS (EnqueueTask, (this, kernel, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1293
		1294	if (ev)
		1295	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1296
		1297	void
		1298	enqueue_nd_range_kernel (OpenCL::Queue this, OpenCL::Kernel kernel, SV *global_work_offset, SV *global_work_size, SV *local_work_size = &PL_sv_undef, ...)
		1299	PPCODE:
		1300	cl_event ev = 0;
		1301	size_t *gwo = 0, *gws, *lws = 0;
		1302	int gws_len;
		1303	size_t *lists;
		1304	int i;
		1305	EVENT_LIST (5, items - 5);
		1306
		1307	if (!SvROK (global_work_size) || SvTYPE (SvRV (global_work_size)) != SVt_PVAV)
		1308	croak ("clEnqueueNDRangeKernel: global_work_size must be an array reference");
		1309
		1310	gws_len = AvFILLp (SvRV (global_work_size)) + 1;
		1311
		1312	lists = tmpbuf (sizeof (size_t) * 3 * gws_len);
		1313
		1314	gws = lists + gws_len * 0;
		1315	for (i = 0; i < gws_len; ++i)
		1316	gws [i] = SvIV (AvARRAY (SvRV (global_work_size))[i]);
		1317
		1318	if (SvOK (global_work_offset))
		1319	{
		1320	if (!SvROK (global_work_offset) || SvTYPE (SvRV (global_work_offset)) != SVt_PVAV)
		1321	croak ("clEnqueueNDRangeKernel: global_work_offset must be undef or an array reference");
		1322
		1323	if (AvFILLp (SvRV (global_work_size)) + 1 != gws_len)
		1324	croak ("clEnqueueNDRangeKernel: global_work_offset must be undef or an array of same size as global_work_size");
		1325
		1326	gwo = lists + gws_len * 1;
		1327	for (i = 0; i < gws_len; ++i)
		1328	gwo [i] = SvIV (AvARRAY (SvRV (global_work_offset))[i]);
		1329	}
		1330
		1331	if (SvOK (local_work_size))
		1332	{
		1333	if (SvOK (local_work_size) && !SvROK (local_work_size) || SvTYPE (SvRV (local_work_size)) != SVt_PVAV)
		1334	croak ("clEnqueueNDRangeKernel: global_work_size must be undef or an array reference");
		1335
		1336	if (AvFILLp (SvRV (local_work_size)) + 1 != gws_len)
		1337	croak ("clEnqueueNDRangeKernel: local_work_local must be undef or an array of same size as global_work_size");
		1338
		1339	lws = lists + gws_len * 2;
		1340	for (i = 0; i < gws_len; ++i)
		1341	lws [i] = SvIV (AvARRAY (SvRV (local_work_size))[i]);
		1342	}
		1343
		1344	NEED_SUCCESS (EnqueueNDRangeKernel, (this, kernel, gws_len, gwo, gws, lws, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1345
		1346	if (ev)
		1347	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1348
		1349	void
		1350	enqueue_marker (OpenCL::Queue this)
		1351	PPCODE:
		1352	cl_event ev;
		1353	NEED_SUCCESS (EnqueueMarker, (this, &ev));
		1354	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1355
		1356	void
		1357	enqueue_wait_for_events (OpenCL::Queue this, ...)
		1358	CODE:
		1359	EVENT_LIST (1, items - 1);
		1360	NEED_SUCCESS (EnqueueWaitForEvents, (this, event_list_count, event_list_ptr));
		1361
		1362	void
		1363	enqueue_barrier (OpenCL::Queue this)
		1364	CODE:
		1365	NEED_SUCCESS (EnqueueBarrier, (this));
		1366
		1367	void
		1368	flush (OpenCL::Queue this)
		1369	CODE:
		1370	NEED_SUCCESS (Flush, (this));
		1371
		1372	void
		1373	finish (OpenCL::Queue this)
		1374	CODE:
		1375	NEED_SUCCESS (Finish, (this));
		1376
		1377	void
		1378	info (OpenCL::Queue this, cl_command_queue_info name)
		1379	PPCODE:
		1380	INFO (CommandQueue)
		1381
		1382	#BEGIN:command_queue
		1383
		1384	void
		1385	context (OpenCL::Queue this)
		1386	PPCODE:
		1387	cl_context value [1];
		1388	NEED_SUCCESS (GetCommandQueueInfo, (this, CL_QUEUE_CONTEXT, sizeof (value), value, 0));
		1389	EXTEND (SP, 1);
		1390	const int i = 0;
		1391	{
		1392	NEED_SUCCESS (RetainContext, (value [i]));
		1393	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1394	}
		1395
		1396	void
		1397	device (OpenCL::Queue this)
		1398	PPCODE:
		1399	cl_device_id value [1];
		1400	NEED_SUCCESS (GetCommandQueueInfo, (this, CL_QUEUE_DEVICE, sizeof (value), value, 0));
		1401	EXTEND (SP, 1);
		1402	const int i = 0;
		1403	{
		1404	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Device", value [i]));
		1405	}
		1406
		1407	void
		1408	reference_count (OpenCL::Queue this)
		1409	PPCODE:
		1410	cl_uint value [1];
		1411	NEED_SUCCESS (GetCommandQueueInfo, (this, CL_QUEUE_REFERENCE_COUNT, sizeof (value), value, 0));
		1412	EXTEND (SP, 1);
		1413	const int i = 0;
		1414	PUSHs (sv_2mortal (newSVuv (value [i])));
		1415
		1416	void
		1417	properties (OpenCL::Queue this)
		1418	PPCODE:
		1419	cl_command_queue_properties value [1];
		1420	NEED_SUCCESS (GetCommandQueueInfo, (this, CL_QUEUE_PROPERTIES, sizeof (value), value, 0));
		1421	EXTEND (SP, 1);
		1422	const int i = 0;
		1423	PUSHs (sv_2mortal (newSViv (value [i])));
		1424
		1425	#END:command_queue
		1426
		1427	MODULE = OpenCL PACKAGE = OpenCL::Memory
		1428
		1429	void
		1430	DESTROY (OpenCL::Memory this)
		1431	CODE:
		1432	clReleaseMemObject (this);
		1433
		1434	void
		1435	info (OpenCL::Memory this, cl_mem_info name)
		1436	PPCODE:
		1437	INFO (MemObject)
		1438
		1439	#BEGIN:mem
		1440
		1441	void
		1442	type (OpenCL::Memory this)
		1443	PPCODE:
		1444	cl_mem_object_type value [1];
		1445	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_TYPE, sizeof (value), value, 0));
		1446	EXTEND (SP, 1);
		1447	const int i = 0;
		1448	PUSHs (sv_2mortal (newSViv (value [i])));
		1449
		1450	void
		1451	flags (OpenCL::Memory this)
		1452	PPCODE:
		1453	cl_mem_flags value [1];
		1454	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_FLAGS, sizeof (value), value, 0));
		1455	EXTEND (SP, 1);
		1456	const int i = 0;
		1457	PUSHs (sv_2mortal (newSViv (value [i])));
		1458
		1459	void
		1460	size (OpenCL::Memory this)
		1461	PPCODE:
		1462	size_t value [1];
		1463	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_SIZE, sizeof (value), value, 0));
		1464	EXTEND (SP, 1);
		1465	const int i = 0;
		1466	PUSHs (sv_2mortal (newSVuv (value [i])));
		1467
		1468	void
		1469	host_ptr (OpenCL::Memory this)
		1470	PPCODE:
		1471	void * value [1];
		1472	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_HOST_PTR, sizeof (value), value, 0));
		1473	EXTEND (SP, 1);
		1474	const int i = 0;
		1475	PUSHs (sv_2mortal (newSVuv ((IV)(intptr_t)value [i])));
		1476
		1477	void
		1478	map_count (OpenCL::Memory this)
		1479	PPCODE:
		1480	cl_uint value [1];
		1481	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_MAP_COUNT, sizeof (value), value, 0));
		1482	EXTEND (SP, 1);
		1483	const int i = 0;
		1484	PUSHs (sv_2mortal (newSVuv (value [i])));
		1485
		1486	void
		1487	reference_count (OpenCL::Memory this)
		1488	PPCODE:
		1489	cl_uint value [1];
		1490	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_REFERENCE_COUNT, sizeof (value), value, 0));
		1491	EXTEND (SP, 1);
		1492	const int i = 0;
		1493	PUSHs (sv_2mortal (newSVuv (value [i])));
		1494
		1495	void
		1496	context (OpenCL::Memory this)
		1497	PPCODE:
		1498	cl_context value [1];
		1499	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_CONTEXT, sizeof (value), value, 0));
		1500	EXTEND (SP, 1);
		1501	const int i = 0;
		1502	{
		1503	NEED_SUCCESS (RetainContext, (value [i]));
		1504	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1505	}
		1506
		1507	void
		1508	associated_memobject (OpenCL::Memory this)
		1509	PPCODE:
		1510	cl_mem value [1];
		1511	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_ASSOCIATED_MEMOBJECT, sizeof (value), value, 0));
		1512	EXTEND (SP, 1);
		1513	const int i = 0;
		1514	{
		1515	NEED_SUCCESS (RetainMemObject, (value [i]));
		1516	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Memory", value [i]));
		1517	}
		1518
		1519	void
		1520	offset (OpenCL::Memory this)
		1521	PPCODE:
		1522	size_t value [1];
		1523	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_OFFSET, sizeof (value), value, 0));
		1524	EXTEND (SP, 1);
		1525	const int i = 0;
		1526	PUSHs (sv_2mortal (newSVuv (value [i])));
		1527
		1528	#END:mem
		1529
		1530	MODULE = OpenCL PACKAGE = OpenCL::Image
		1531
		1532	void
		1533	image_info (OpenCL::Image this, cl_image_info name)
		1534	PPCODE:
		1535	INFO (Image)
		1536
		1537	#BEGIN:image
		1538
		1539	void
		1540	element_size (OpenCL::Image this)
		1541	PPCODE:
		1542	size_t value [1];
		1543	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_ELEMENT_SIZE, sizeof (value), value, 0));
		1544	EXTEND (SP, 1);
		1545	const int i = 0;
		1546	PUSHs (sv_2mortal (newSVuv (value [i])));
		1547
		1548	void
		1549	row_pitch (OpenCL::Image this)
		1550	PPCODE:
		1551	size_t value [1];
		1552	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_ROW_PITCH, sizeof (value), value, 0));
		1553	EXTEND (SP, 1);
		1554	const int i = 0;
		1555	PUSHs (sv_2mortal (newSVuv (value [i])));
		1556
		1557	void
		1558	slice_pitch (OpenCL::Image this)
		1559	PPCODE:
		1560	size_t value [1];
		1561	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_SLICE_PITCH, sizeof (value), value, 0));
		1562	EXTEND (SP, 1);
		1563	const int i = 0;
		1564	PUSHs (sv_2mortal (newSVuv (value [i])));
		1565
		1566	void
		1567	width (OpenCL::Image this)
		1568	PPCODE:
		1569	size_t value [1];
		1570	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_WIDTH, sizeof (value), value, 0));
		1571	EXTEND (SP, 1);
		1572	const int i = 0;
		1573	PUSHs (sv_2mortal (newSVuv (value [i])));
		1574
		1575	void
		1576	height (OpenCL::Image this)
		1577	PPCODE:
		1578	size_t value [1];
		1579	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_HEIGHT, sizeof (value), value, 0));
		1580	EXTEND (SP, 1);
		1581	const int i = 0;
		1582	PUSHs (sv_2mortal (newSVuv (value [i])));
		1583
		1584	void
		1585	depth (OpenCL::Image this)
		1586	PPCODE:
		1587	size_t value [1];
		1588	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_DEPTH, sizeof (value), value, 0));
		1589	EXTEND (SP, 1);
		1590	const int i = 0;
		1591	PUSHs (sv_2mortal (newSVuv (value [i])));
		1592
		1593	#END:image
		1594
		1595	MODULE = OpenCL PACKAGE = OpenCL::Sampler
		1596
		1597	void
		1598	DESTROY (OpenCL::Sampler this)
		1599	CODE:
		1600	clReleaseSampler (this);
		1601
		1602	void
		1603	info (OpenCL::Sampler this, cl_sampler_info name)
		1604	PPCODE:
		1605	INFO (Sampler)
		1606
		1607	#BEGIN:sampler
		1608
		1609	void
		1610	reference_count (OpenCL::Sampler this)
		1611	PPCODE:
		1612	cl_uint value [1];
		1613	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_REFERENCE_COUNT, sizeof (value), value, 0));
		1614	EXTEND (SP, 1);
		1615	const int i = 0;
		1616	PUSHs (sv_2mortal (newSVuv (value [i])));
		1617
		1618	void
		1619	context (OpenCL::Sampler this)
		1620	PPCODE:
		1621	cl_context value [1];
		1622	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_CONTEXT, sizeof (value), value, 0));
		1623	EXTEND (SP, 1);
		1624	const int i = 0;
		1625	{
		1626	NEED_SUCCESS (RetainContext, (value [i]));
		1627	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1628	}
		1629
		1630	void
		1631	normalized_coords (OpenCL::Sampler this)
		1632	PPCODE:
		1633	cl_addressing_mode value [1];
		1634	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_NORMALIZED_COORDS, sizeof (value), value, 0));
		1635	EXTEND (SP, 1);
		1636	const int i = 0;
		1637	PUSHs (sv_2mortal (newSViv (value [i])));
		1638
		1639	void
		1640	addressing_mode (OpenCL::Sampler this)
		1641	PPCODE:
		1642	cl_filter_mode value [1];
		1643	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_ADDRESSING_MODE, sizeof (value), value, 0));
		1644	EXTEND (SP, 1);
		1645	const int i = 0;
		1646	PUSHs (sv_2mortal (newSViv (value [i])));
		1647
		1648	void
		1649	filter_mode (OpenCL::Sampler this)
		1650	PPCODE:
		1651	cl_bool value [1];
		1652	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_FILTER_MODE, sizeof (value), value, 0));
		1653	EXTEND (SP, 1);
		1654	const int i = 0;
		1655	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		1656
		1657	#END:sampler
		1658
94	MODULE = OpenCL PACKAGE = OpenCL::Platform	1659	MODULE = OpenCL PACKAGE = OpenCL::Program
95		1660
96	void	1661	void
97	info (OpenCL::Platform this, cl_platform_info name)	1662	DESTROY (OpenCL::Program this)
98	PPCODE:	1663	CODE:
99	{	1664	clReleaseProgram (this);
		1665
		1666	void
		1667	build (OpenCL::Program this, OpenCL::Device device, SV *options = &PL_sv_undef)
		1668	CODE:
		1669	NEED_SUCCESS (BuildProgram, (this, 1, &device, SvPVbyte_nolen (options), 0, 0));
		1670
		1671	void
		1672	build_info (OpenCL::Program this, OpenCL::Device device, cl_program_build_info name)
		1673	PPCODE:
100	size_t size;	1674	size_t size;
101	SV *sv;
102
103	NEED_SUCCESS (clGetPlatformInfo, (this, name, 0, 0, &size));	1675	NEED_SUCCESS (GetProgramBuildInfo, (this, device, name, 0, 0, &size));
104	sv = sv_2mortal (newSV (size));	1676	SV *sv = sv_2mortal (newSV (size));
105	SvUPGRADE (sv, SVt_PV);	1677	SvUPGRADE (sv, SVt_PV);
106	SvPOK_only (sv);	1678	SvPOK_only (sv);
107	SvCUR_set (sv, size);	1679	SvCUR_set (sv, size);
108	NEED_SUCCESS (clGetPlatformInfo, (this, name, size, SvPVX (sv), 0));	1680	NEED_SUCCESS (GetProgramBuildInfo, (this, device, name, size, SvPVX (sv), 0));
109	XPUSHs (sv);	1681	XPUSHs (sv);
110	}
111		1682
		1683	#BEGIN:program_build
		1684
112	void	1685	void
113	devices (OpenCL::Platform this, cl_device_type type = CL_DEVICE_TYPE_ALL)	1686	build_status (OpenCL::Program this, OpenCL::Device device)
114	PPCODE:	1687	PPCODE:
115	{	1688	cl_build_status value [1];
116	cl_device_id *list;	1689	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_STATUS, sizeof (value), value, 0));
		1690	EXTEND (SP, 1);
		1691	const int i = 0;
		1692	PUSHs (sv_2mortal (newSViv (value [i])));
		1693
		1694	void
		1695	build_options (OpenCL::Program this, OpenCL::Device device)
		1696	PPCODE:
		1697	size_t size;
		1698	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_OPTIONS, 0, 0, &size));
		1699	char *value = tmpbuf (size);
		1700	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_OPTIONS, size, value, 0));
		1701	int i, n = 1;
		1702	EXTEND (SP, n);
		1703	for (i = 0; i < n; ++i)
		1704	PUSHs (sv_2mortal (newSVpv (value, 0)));
		1705
		1706	void
		1707	build_log (OpenCL::Program this, OpenCL::Device device)
		1708	PPCODE:
		1709	size_t size;
		1710	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_LOG, 0, 0, &size));
		1711	char *value = tmpbuf (size);
		1712	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_LOG, size, value, 0));
		1713	int i, n = 1;
		1714	EXTEND (SP, n);
		1715	for (i = 0; i < n; ++i)
		1716	PUSHs (sv_2mortal (newSVpv (value, 0)));
		1717
		1718	#END:program_build
		1719
		1720	void
		1721	kernel (OpenCL::Program program, SV *function)
		1722	PPCODE:
		1723	NEED_SUCCESS_ARG (cl_kernel kernel, CreateKernel, (program, SvPVbyte_nolen (function), &res));
		1724	XPUSH_NEW_OBJ ("OpenCL::Kernel", kernel);
		1725
		1726	void
		1727	info (OpenCL::Program this, cl_program_info name)
		1728	PPCODE:
		1729	INFO (Program)
		1730
		1731	void
		1732	binaries (OpenCL::Program this)
		1733	PPCODE:
117	cl_uint count;	1734	cl_uint n, i;
118	int i;	1735	size_t size;
119		1736
120	NEED_SUCCESS (clGetDeviceIDs, (this, type, 0, 0, &count));	1737	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_NUM_DEVICES , sizeof (n) , &n , 0));
121	Newx (list, count, cl_device_id);	1738	if (!n) XSRETURN_EMPTY;
122	NEED_SUCCESS (clGetDeviceIDs, (this, type, count, list, 0));
123		1739
		1740	size_t *sizes = tmpbuf (sizeof (*sizes) * n);
		1741	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_BINARY_SIZES, sizeof (*sizes) * n, sizes, &size));
		1742	if (size != sizeof (*sizes) * n) XSRETURN_EMPTY;
		1743	unsigned char **ptrs = tmpbuf (sizeof (*ptrs) * n);
		1744
124	EXTEND (SP, count);	1745	EXTEND (SP, n);
125	for (i = 0; i < count; ++i)	1746	for (i = 0; i < n; ++i)
126	PUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Device", list [i]));	1747	{
		1748	SV *sv = sv_2mortal (newSV (sizes [i]));
		1749	SvUPGRADE (sv, SVt_PV);
		1750	SvPOK_only (sv);
		1751	SvCUR_set (sv, sizes [i]);
		1752	ptrs [i] = SvPVX (sv);
		1753	PUSHs (sv);
		1754	}
127		1755
128	Safefree (list);	1756	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_BINARIES , sizeof (*ptrs ) * n, ptrs , &size));
129	}	1757	if (size != sizeof (*ptrs) * n) XSRETURN_EMPTY;
130		1758
		1759	#BEGIN:program
		1760
131	void	1761	void
132	context_from_type_simple (OpenCL::Platform this, cl_device_type type = CL_DEVICE_TYPE_DEFAULT)	1762	reference_count (OpenCL::Program this)
133	PPCODE:	1763	PPCODE:
134	{	1764	cl_uint value [1];
135	cl_int res;	1765	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_REFERENCE_COUNT, sizeof (value), value, 0));
136	cl_context_properties props[] = { CL_CONTEXT_PLATFORM, (cl_context_properties)this, 0 };	1766	EXTEND (SP, 1);
137	cl_context ctx = clCreateContextFromType (props, type, 0, 0, &res);	1767	const int i = 0;
		1768	PUSHs (sv_2mortal (newSVuv (value [i])));
138		1769
139	if (res)	1770	void
140	FAIL (clCreateContextFromType, res);	1771	context (OpenCL::Program this)
		1772	PPCODE:
		1773	cl_context value [1];
		1774	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_CONTEXT, sizeof (value), value, 0));
		1775	EXTEND (SP, 1);
		1776	const int i = 0;
		1777	{
		1778	NEED_SUCCESS (RetainContext, (value [i]));
		1779	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1780	}
141		1781
142	XPUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Context", ctx));	1782	void
143	}	1783	num_devices (OpenCL::Program this)
		1784	PPCODE:
		1785	cl_uint value [1];
		1786	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_NUM_DEVICES, sizeof (value), value, 0));
		1787	EXTEND (SP, 1);
		1788	const int i = 0;
		1789	PUSHs (sv_2mortal (newSVuv (value [i])));
144		1790
		1791	void
		1792	devices (OpenCL::Program this)
		1793	PPCODE:
		1794	size_t size;
		1795	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_DEVICES, 0, 0, &size));
		1796	cl_device_id *value = tmpbuf (size);
		1797	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_DEVICES, size, value, 0));
		1798	int i, n = size / sizeof (*value);
		1799	EXTEND (SP, n);
		1800	for (i = 0; i < n; ++i)
		1801	{
		1802	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Device", value [i]));
		1803	}
		1804
		1805	void
		1806	source (OpenCL::Program this)
		1807	PPCODE:
		1808	size_t size;
		1809	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_SOURCE, 0, 0, &size));
		1810	char *value = tmpbuf (size);
		1811	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_SOURCE, size, value, 0));
		1812	int i, n = 1;
		1813	EXTEND (SP, n);
		1814	for (i = 0; i < n; ++i)
		1815	PUSHs (sv_2mortal (newSVpv (value, 0)));
		1816
		1817	void
		1818	binary_sizes (OpenCL::Program this)
		1819	PPCODE:
		1820	size_t size;
		1821	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_BINARY_SIZES, 0, 0, &size));
		1822	size_t *value = tmpbuf (size);
		1823	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_BINARY_SIZES, size, value, 0));
		1824	int i, n = size / sizeof (*value);
		1825	EXTEND (SP, n);
		1826	for (i = 0; i < n; ++i)
		1827	PUSHs (sv_2mortal (newSVuv (value [i])));
		1828
		1829	#END:program
		1830
145	MODULE = OpenCL PACKAGE = OpenCL::Device	1831	MODULE = OpenCL PACKAGE = OpenCL::Kernel
146		1832
147	void	1833	void
		1834	DESTROY (OpenCL::Kernel this)
		1835	CODE:
		1836	clReleaseKernel (this);
		1837
		1838	void
		1839	set_char (OpenCL::Kernel this, cl_uint idx, cl_char value)
		1840	CODE:
		1841	clSetKernelArg (this, idx, sizeof (value), &value);
		1842
		1843	void
		1844	set_uchar (OpenCL::Kernel this, cl_uint idx, cl_uchar value)
		1845	CODE:
		1846	clSetKernelArg (this, idx, sizeof (value), &value);
		1847
		1848	void
		1849	set_short (OpenCL::Kernel this, cl_uint idx, cl_short value)
		1850	CODE:
		1851	clSetKernelArg (this, idx, sizeof (value), &value);
		1852
		1853	void
		1854	set_ushort (OpenCL::Kernel this, cl_uint idx, cl_ushort value)
		1855	CODE:
		1856	clSetKernelArg (this, idx, sizeof (value), &value);
		1857
		1858	void
		1859	set_int (OpenCL::Kernel this, cl_uint idx, cl_int value)
		1860	CODE:
		1861	clSetKernelArg (this, idx, sizeof (value), &value);
		1862
		1863	void
		1864	set_uint (OpenCL::Kernel this, cl_uint idx, cl_uint value)
		1865	CODE:
		1866	clSetKernelArg (this, idx, sizeof (value), &value);
		1867
		1868	void
		1869	set_long (OpenCL::Kernel this, cl_uint idx, cl_long value)
		1870	CODE:
		1871	clSetKernelArg (this, idx, sizeof (value), &value);
		1872
		1873	void
		1874	set_ulong (OpenCL::Kernel this, cl_uint idx, cl_ulong value)
		1875	CODE:
		1876	clSetKernelArg (this, idx, sizeof (value), &value);
		1877
		1878	void
		1879	set_half (OpenCL::Kernel this, cl_uint idx, cl_half value)
		1880	CODE:
		1881	clSetKernelArg (this, idx, sizeof (value), &value);
		1882
		1883	void
		1884	set_float (OpenCL::Kernel this, cl_uint idx, cl_float value)
		1885	CODE:
		1886	clSetKernelArg (this, idx, sizeof (value), &value);
		1887
		1888	void
		1889	set_double (OpenCL::Kernel this, cl_uint idx, cl_double value)
		1890	CODE:
		1891	clSetKernelArg (this, idx, sizeof (value), &value);
		1892
		1893	void
		1894	set_memory (OpenCL::Kernel this, cl_uint idx, OpenCL::Memory_ornull value)
		1895	CODE:
		1896	clSetKernelArg (this, idx, sizeof (value), &value);
		1897
		1898	void
		1899	set_buffer (OpenCL::Kernel this, cl_uint idx, OpenCL::Buffer_ornull value)
		1900	CODE:
		1901	clSetKernelArg (this, idx, sizeof (value), &value);
		1902
		1903	void
		1904	set_image2d (OpenCL::Kernel this, cl_uint idx, OpenCL::Image2D_ornull value)
		1905	CODE:
		1906	clSetKernelArg (this, idx, sizeof (value), &value);
		1907
		1908	void
		1909	set_image3d (OpenCL::Kernel this, cl_uint idx, OpenCL::Image3D_ornull value)
		1910	CODE:
		1911	clSetKernelArg (this, idx, sizeof (value), &value);
		1912
		1913	void
		1914	set_sampler (OpenCL::Kernel this, cl_uint idx, OpenCL::Sampler value)
		1915	CODE:
		1916	clSetKernelArg (this, idx, sizeof (value), &value);
		1917
		1918	void
		1919	set_event (OpenCL::Kernel this, cl_uint idx, OpenCL::Event value)
		1920	CODE:
		1921	clSetKernelArg (this, idx, sizeof (value), &value);
		1922
		1923	void
148	info (OpenCL::Device this, cl_device_info name)	1924	info (OpenCL::Kernel this, cl_kernel_info name)
		1925	PPCODE:
		1926	INFO (Kernel)
		1927
		1928	#BEGIN:kernel
		1929
		1930	void
		1931	function_name (OpenCL::Kernel this)
149	PPCODE:	1932	PPCODE:
150	{	1933	size_t size;
		1934	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_FUNCTION_NAME, 0, 0, &size));
		1935	char *value = tmpbuf (size);
		1936	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_FUNCTION_NAME, size, value, 0));
		1937	int i, n = 1;
		1938	EXTEND (SP, n);
		1939	for (i = 0; i < n; ++i)
		1940	PUSHs (sv_2mortal (newSVpv (value, 0)));
		1941
		1942	void
		1943	num_args (OpenCL::Kernel this)
		1944	PPCODE:
		1945	cl_uint value [1];
		1946	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_NUM_ARGS, sizeof (value), value, 0));
		1947	EXTEND (SP, 1);
		1948	const int i = 0;
		1949	PUSHs (sv_2mortal (newSVuv (value [i])));
		1950
		1951	void
		1952	reference_count (OpenCL::Kernel this)
		1953	PPCODE:
		1954	cl_uint value [1];
		1955	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_REFERENCE_COUNT, sizeof (value), value, 0));
		1956	EXTEND (SP, 1);
		1957	const int i = 0;
		1958	PUSHs (sv_2mortal (newSVuv (value [i])));
		1959
		1960	void
		1961	context (OpenCL::Kernel this)
		1962	PPCODE:
		1963	cl_context value [1];
		1964	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_CONTEXT, sizeof (value), value, 0));
		1965	EXTEND (SP, 1);
		1966	const int i = 0;
		1967	{
		1968	NEED_SUCCESS (RetainContext, (value [i]));
		1969	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1970	}
		1971
		1972	void
		1973	program (OpenCL::Kernel this)
		1974	PPCODE:
		1975	cl_program value [1];
		1976	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_PROGRAM, sizeof (value), value, 0));
		1977	EXTEND (SP, 1);
		1978	const int i = 0;
		1979	{
		1980	NEED_SUCCESS (RetainProgram, (value [i]));
		1981	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Program", value [i]));
		1982	}
		1983
		1984	#END:kernel
		1985
		1986	void
		1987	work_group_info (OpenCL::Kernel this, OpenCL::Device device, cl_kernel_work_group_info name)
		1988	PPCODE:
151	size_t size;	1989	size_t size;
152	SV *sv;
153
154	NEED_SUCCESS (clGetDeviceInfo, (this, name, 0, 0, &size));	1990	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, name, 0, 0, &size));
155	sv = sv_2mortal (newSV (size));	1991	SV *sv = sv_2mortal (newSV (size));
156	SvUPGRADE (sv, SVt_PV);	1992	SvUPGRADE (sv, SVt_PV);
157	SvPOK_only (sv);	1993	SvPOK_only (sv);
158	SvCUR_set (sv, size);	1994	SvCUR_set (sv, size);
159	NEED_SUCCESS (clGetDeviceInfo, (this, name, size, SvPVX (sv), 0));	1995	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, name, size, SvPVX (sv), 0));
160	XPUSHs (sv);	1996	XPUSHs (sv);
161	}
162		1997
		1998	#BEGIN:kernel_work_group
		1999
163	void	2000	void
164	context_simple (OpenCL::Device this)	2001	work_group_size (OpenCL::Kernel this, OpenCL::Device device)
165	PPCODE:	2002	PPCODE:
166	{	2003	size_t value [1];
167	cl_int res;	2004	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_WORK_GROUP_SIZE, sizeof (value), value, 0));
168	cl_context ctx = clCreateContext (0, 1, &this, 0, 0, &res);	2005	EXTEND (SP, 1);
		2006	const int i = 0;
		2007	PUSHs (sv_2mortal (newSVuv (value [i])));
169		2008
170	if (res)
171	FAIL (clCreateContext, res);
172
173	XPUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Context", ctx));
174	}
175
176	MODULE = OpenCL PACKAGE = OpenCL::Context
177
178	void	2009	void
179	DESTROY (OpenCL::Context context)	2010	compile_work_group_size (OpenCL::Kernel this, OpenCL::Device device)
180	CODE:
181	clReleaseContext (context);
182
183	void
184	info (OpenCL::Context this, cl_context_info name)
185	PPCODE:	2011	PPCODE:
186	{
187	size_t size;	2012	size_t size;
188	SV *sv;	2013	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_COMPILE_WORK_GROUP_SIZE, 0, 0, &size));
		2014	size_t *value = tmpbuf (size);
		2015	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_COMPILE_WORK_GROUP_SIZE, size, value, 0));
		2016	int i, n = size / sizeof (*value);
		2017	EXTEND (SP, n);
		2018	for (i = 0; i < n; ++i)
		2019	PUSHs (sv_2mortal (newSVuv (value [i])));
189		2020
190	NEED_SUCCESS (clGetContextInfo, (this, name, 0, 0, &size));
191	sv = sv_2mortal (newSV (size));
192	SvUPGRADE (sv, SVt_PV);
193	SvPOK_only (sv);
194	SvCUR_set (sv, size);
195	NEED_SUCCESS (clGetContextInfo, (this, name, size, SvPVX (sv), 0));
196	XPUSHs (sv);
197	}
198
199	void	2021	void
200	command_queue_simple (OpenCL::Context this, OpenCL::Device device)	2022	local_mem_size (OpenCL::Kernel this, OpenCL::Device device)
201	PPCODE:	2023	PPCODE:
202	{	2024	cl_ulong value [1];
203	cl_int res;	2025	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_LOCAL_MEM_SIZE, sizeof (value), value, 0));
204	cl_command_queue queue = clCreateCommandQueue (this, device, 0, &res);	2026	EXTEND (SP, 1);
		2027	const int i = 0;
		2028	PUSHs (sv_2mortal (newSVuv (value [i])));
205		2029
206	if (res)	2030	void
207	FAIL (clCreateCommandQueue, res);	2031	preferred_work_group_size_multiple (OpenCL::Kernel this, OpenCL::Device device)
		2032	PPCODE:
		2033	size_t value [1];
		2034	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE, sizeof (value), value, 0));
		2035	EXTEND (SP, 1);
		2036	const int i = 0;
		2037	PUSHs (sv_2mortal (newSVuv (value [i])));
208		2038
209	XPUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Queue", queue));	2039	void
210	}	2040	private_mem_size (OpenCL::Kernel this, OpenCL::Device device)
		2041	PPCODE:
		2042	cl_ulong value [1];
		2043	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_PRIVATE_MEM_SIZE, sizeof (value), value, 0));
		2044	EXTEND (SP, 1);
		2045	const int i = 0;
		2046	PUSHs (sv_2mortal (newSVuv (value [i])));
211		2047
		2048	#END:kernel_work_group
		2049
212	MODULE = OpenCL PACKAGE = OpenCL::Queue	2050	MODULE = OpenCL PACKAGE = OpenCL::Event
213		2051
214	void	2052	void
215	DESTROY (OpenCL::Queue this)	2053	DESTROY (OpenCL::Event this)
		2054	CODE:
		2055	clReleaseEvent (this);
		2056
		2057	void
		2058	wait (OpenCL::Event this)
		2059	CODE:
		2060	clWaitForEvents (1, &this);
		2061
		2062	void
		2063	info (OpenCL::Event this, cl_event_info name)
216	CODE:	2064	PPCODE:
217	clReleaseCommandQueue (this);	2065	INFO (Event)
218		2066
		2067	#BEGIN:event
		2068
219	void	2069	void
220	info (OpenCL::Queue this, cl_command_queue_info name)	2070	command_queue (OpenCL::Event this)
221	PPCODE:	2071	PPCODE:
222	{	2072	cl_command_queue value [1];
223	size_t size;	2073	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_COMMAND_QUEUE, sizeof (value), value, 0));
224	SV *sv;	2074	EXTEND (SP, 1);
		2075	const int i = 0;
		2076	{
		2077	NEED_SUCCESS (RetainCommandQueue, (value [i]));
		2078	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Queue", value [i]));
		2079	}
225		2080
226	NEED_SUCCESS (clGetCommandQueueInfo, (this, name, 0, 0, &size));	2081	void
227	sv = sv_2mortal (newSV (size));	2082	command_type (OpenCL::Event this)
228	SvUPGRADE (sv, SVt_PV);	2083	PPCODE:
229	SvPOK_only (sv);	2084	cl_command_type value [1];
230	SvCUR_set (sv, size);	2085	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_COMMAND_TYPE, sizeof (value), value, 0));
231	NEED_SUCCESS (clGetCommandQueueInfo, (this, name, size, SvPVX (sv), 0));	2086	EXTEND (SP, 1);
232	XPUSHs (sv);	2087	const int i = 0;
233	}	2088	PUSHs (sv_2mortal (newSVuv (value [i])));
234		2089
		2090	void
		2091	reference_count (OpenCL::Event this)
		2092	PPCODE:
		2093	cl_uint value [1];
		2094	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_REFERENCE_COUNT, sizeof (value), value, 0));
		2095	EXTEND (SP, 1);
		2096	const int i = 0;
		2097	PUSHs (sv_2mortal (newSVuv (value [i])));
		2098
		2099	void
		2100	command_execution_status (OpenCL::Event this)
		2101	PPCODE:
		2102	cl_uint value [1];
		2103	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_COMMAND_EXECUTION_STATUS, sizeof (value), value, 0));
		2104	EXTEND (SP, 1);
		2105	const int i = 0;
		2106	PUSHs (sv_2mortal (newSVuv (value [i])));
		2107
		2108	void
		2109	context (OpenCL::Event this)
		2110	PPCODE:
		2111	cl_context value [1];
		2112	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_CONTEXT, sizeof (value), value, 0));
		2113	EXTEND (SP, 1);
		2114	const int i = 0;
		2115	{
		2116	NEED_SUCCESS (RetainContext, (value [i]));
		2117	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		2118	}
		2119
		2120	#END:event
		2121
		2122	void
		2123	profiling_info (OpenCL::Event this, cl_profiling_info name)
		2124	PPCODE:
		2125	INFO (EventProfiling)
		2126
		2127	#BEGIN:profiling
		2128
		2129	void
		2130	profiling_command_queued (OpenCL::Event this)
		2131	PPCODE:
		2132	cl_ulong value [1];
		2133	NEED_SUCCESS (GetEventProfilingInfo, (this, CL_PROFILING_COMMAND_QUEUED, sizeof (value), value, 0));
		2134	EXTEND (SP, 1);
		2135	const int i = 0;
		2136	PUSHs (sv_2mortal (newSVuv (value [i])));
		2137
		2138	void
		2139	profiling_command_submit (OpenCL::Event this)
		2140	PPCODE:
		2141	cl_ulong value [1];
		2142	NEED_SUCCESS (GetEventProfilingInfo, (this, CL_PROFILING_COMMAND_SUBMIT, sizeof (value), value, 0));
		2143	EXTEND (SP, 1);
		2144	const int i = 0;
		2145	PUSHs (sv_2mortal (newSVuv (value [i])));
		2146
		2147	void
		2148	profiling_command_start (OpenCL::Event this)
		2149	PPCODE:
		2150	cl_ulong value [1];
		2151	NEED_SUCCESS (GetEventProfilingInfo, (this, CL_PROFILING_COMMAND_START, sizeof (value), value, 0));
		2152	EXTEND (SP, 1);
		2153	const int i = 0;
		2154	PUSHs (sv_2mortal (newSVuv (value [i])));
		2155
		2156	void
		2157	profiling_command_end (OpenCL::Event this)
		2158	PPCODE:
		2159	cl_ulong value [1];
		2160	NEED_SUCCESS (GetEventProfilingInfo, (this, CL_PROFILING_COMMAND_END, sizeof (value), value, 0));
		2161	EXTEND (SP, 1);
		2162	const int i = 0;
		2163	PUSHs (sv_2mortal (newSVuv (value [i])));
		2164
		2165	#END:profiling
		2166
		2167	MODULE = OpenCL PACKAGE = OpenCL::UserEvent
		2168
		2169	void
		2170	set_status (OpenCL::UserEvent this, cl_int execution_status)
		2171	CODE:
		2172	clSetUserEventStatus (this, execution_status);
		2173

Diff Legend

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