Initial commit

author: Thomas Albers <thomas@thomaslabs.org> 2023-03-04 22:47:28 +0100
committer: Thomas Albers <thomas@thomaslabs.org> 2023-03-04 22:47:28 +0100
commit: 6fe823a614279cceb2d48507bd8e93b0efd87f94 (patch)
tree: 579e3c5db456667ce2aeda94f909703513179ce1 /src
19 files changed, 3048 insertions, 0 deletions
diff --git a/src/bindings.lisp b/src/bindings.lisp
new file mode 100644
index 0000000..0cc08ba
--- /dev/null
+++ b/src/bindings.lisp
@@ -0,0 +1,832 @@
+(in-package #:ocl-ffi)
+
+;;; Platform API
+
+(cffi:defcfun ("clGetPlatformIDs" %get-platform-ids) cl-error-code
+  (num-entries cl-uint)
+  (platforms cl-platform-id)
+  (num-platforms (:pointer cl-uint)))
+
+(cffi:defcfun ("clGetPlatformInfo" %get-platform-info) cl-error-code
+  (platform cl-platform-id)
+  (param-name cl-platform-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+;;; Device APIs
+
+(cffi:defcfun ("clGetDeviceIDs" %get-device-ids) cl-error-code
+  (platform cl-platform-id)
+  (device-type cl-device-type)
+  (num-entries cl-uint)
+  (devices (:pointer cl-device-id))
+  (num-devices (:pointer cl-uint)))
+
+(cffi:defcfun ("clGetDeviceInfo" %get-device-info) cl-error-code
+  (device cl-device-id)
+  (param-name cl-device-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clCreateSubDevices" %create-sub-devices) cl-int
+  (in-device cl-device-id)
+  (properties (:pointer cl-device-partition-property))
+  (num-devices cl-uint)
+  (out-devices (:pointer cl-device-id))
+  (num-devices-ret (:pointer cl-uint)))
+
+(cffi:defcfun ("clRetainDevice" %retain-device) cl-error-code
+  (device cl-device-id))
+
+(cffi:defcfun ("clReleaseDevice" %release-device) cl-error-code
+  (device cl-device-id))
+
+(cffi:defcfun ("clSetDefaultDeviceCommandQueue" %set-default-device-command-queue) cl-int
+  (context cl-context)
+  (device cl-device-id)
+  (command-queue cl-command-queue))
+
+(cffi:defcfun ("clGetDeviceAndHostTimer" %get-device-and-host-timer) cl-int
+  (device cl-device-id)
+  (device-timestamp (:pointer cl-ulong))
+  (host-timestamp (:pointer cl-ulong)))
+
+(cffi:defcfun ("clGetHostTimer" %get-host-timer) cl-int
+  (device cl-device-id)
+  (host-timestamp (:pointer cl-ulong)))
+
+;;; Context APIs
+
+(cffi:defcfun ("clCreateContext" %create-context) cl-context
+  (properties (:pointer cl-context-properties))
+  (num-devices cl-uint)
+  (devices (:pointer cl-device-id))
+  (pfn-notify :pointer)
+  (user-data (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateContextFromType" %create-context-from-type) cl-context
+  (device-type cl-device-type)
+  (pfn-notify :pointer)
+  (user-data (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clRetainContext" %retain-context) cl-error-code
+  (context cl-context))
+
+(cffi:defcfun ("clReleaseContext" %release-context) cl-error-code
+  (context cl-context))
+
+(cffi:defcfun ("clGetContextInfo" %get-context-info) cl-int
+  (context cl-context)
+  (param-name cl-context-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clSetContextDestructorCallback" set-context-destructor-callback) cl-int
+  (context cl-context)
+  (pfn-notify :pointer)
+  (user-data (:pointer :void)))
+
+;;; Command Queue APIs
+
+(cffi:defcfun ("clCreateCommandQueueWithProperties" %create-command-queue-with-properties) cl-command-queue
+  (context cl-context)
+  (device cl-device-id)
+  (properties (:pointer cl-queue-properties))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clRetainCommandQueue" %retain-command-queue) cl-error-code
+  (command-queue cl-command-queue))
+
+(cffi:defcfun ("clReleaseCommandQueue" %release-command-queue) cl-error-code
+  (command-queue cl-command-queue))
+
+(cffi:defcfun ("clGetCommandQueueInfo" %get-command-queue-info) cl-int
+  (command-queue cl-command-queue)
+  (param-name cl-command-queue-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+;;; Memory Object APIs
+
+(cffi:defcfun ("clCreateBuffer" %create-buffer) cl-mem
+  (context cl-context)
+  (flags cl-mem-flags)
+  (size :size)
+  (host-ptr (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateSubBuffer" create-sub-buffer) cl-mem
+  (buffer cl-mem)
+  (flags cl-mem-flags)
+  (size :size)
+  (host-ptr (:pointer :void))
+  (buffer-create-type cl-buffer-create-type)
+  (buffer-create-info (:pointer :void))
+  (errcode-ret (:pointer :int)))
+
+(cffi:defcfun ("clCreateImage" create-image) cl-mem
+  (context cl-context)
+  (flags cl-mem-flags)
+  (image-format (:pointer (:struct cl-image-format)))
+  (image-desc (:pointer (:struct cl-image-desc)))
+  (host-ptr (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreatePipe" %create-pipe) cl-mem
+  (context cl-context)
+  (flags cl-mem-flags)
+  (pipe-packet-size cl-uint)
+  (pipe-max-packets cl-uint)
+  (properties (:pointer cl-pipe-properties))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateBufferWithProperties" create-buffer-with-properties) cl-mem
+  (context cl-context)
+  (properties (:pointer cl-mem-properties))
+  (flags cl-mem-flags)
+  (size :size)
+  (host-ptr (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateImageWithProperties" create-image-with-properties) cl-mem
+  (context cl-context)
+  (properties (:pointer cl-mem-properties))
+  (flags cl-mem-flags)
+  (image-format (:pointer (:struct cl-image-format)))
+  (image-desc (:pointer (:struct cl-image-desc)))
+  (host-ptr (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clRetainMemObject" %retain-mem-object) cl-error-code
+  (memobj cl-mem))
+
+(cffi:defcfun ("clReleaseMemObject" %release-mem-object) cl-error-code
+  (memobj cl-mem))
+
+(cffi:defcfun ("clGetSupportedImageFormats" %get-supported-image-formats) cl-error-code
+  (context cl-context)
+  (flags cl-mem-flags)
+  (image-type cl-mem-object-type)
+  (num-entries cl-uint)
+  (image-formats (:pointer (:struct cl-image-format)))
+  (num-image-formats (:pointer cl-uint)))
+
+(cffi:defcfun ("clGetMemObjectInfo" %get-mem-object-info) cl-int
+  (memobj cl-mem)
+  (param-name cl-mem-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clGetImageInfo" %get-image-info) cl-int
+  (image cl-mem)
+  (param-name cl-image-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clGetPipeInfo" %get-pipe-info) cl-int
+  (pipe cl-mem)
+  (param-name cl-pipe-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clSetMemObjectDestructorCallback" set-mem-object-destructor-callback) cl-int
+  (memobj cl-mem)
+  (pfn-notify :pointer)
+  (user-data (:pointer :void)))
+
+;;; SVM Allocation APIs
+
+(cffi:defcfun ("clSVMAlloc" svm-alloc) (:pointer :void)
+  (context cl-context)
+  (flags cl-svm-mem-flags)
+  (size :size)
+  (aligment cl-uint))
+
+(cffi:defcfun ("clSVMFree" svm-free) :void
+  (context cl-context)
+  (svm-pointer (:pointer :void)))
+
+;;; Sampler APIs
+
+(cffi:defcfun ("clCreateSamplerWithProperties" %create-sampler-with-properties) cl-sampler
+  (context cl-context)
+  (sampler-properties (:pointer cl-sampler-properties))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clRetainSampler" %retain-sampler) cl-int
+  (sampler cl-sampler))
+
+(cffi:defcfun ("clReleaseSampler" %release-sampler) cl-int
+  (sampler cl-sampler))
+
+(cffi:defcfun ("clGetSamplerInfo" %get-sampler-info) cl-int
+  (sampler cl-sampler)
+  (param-name cl-sampler-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+;;; Program Object APIs
+
+(cffi:defcfun ("clCreateProgramWithSource" %create-program-with-source) cl-program
+  (context cl-context)
+  (count cl-uint)
+  (strings (:pointer (:pointer :char)))
+  (lengths (:pointer :size))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateProgramWithBinary" create-program-with-binary) cl-program
+  (context cl-context)
+  (num-devices cl-uint)
+  (device-list (:pointer cl-device-id))
+  (lengths (:pointer :size))
+  (binaries (:pointer (:pointer :unsigned-char)))
+  (binary-status (:pointer cl-int))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateProgramWithBuiltInKernels" create-program-with-built-in-kernels) cl-program
+  (context cl-context)
+  (num-devices cl-uint)
+  (device-list (:pointer cl-device-id))
+  (kernel-names (:pointer :char))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateProgramWithIL" create-program-with-il) cl-program
+  (context cl-context)
+  (il (:pointer :void))
+  (length :size)
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clRetainProgram" %retain-program) cl-error-code
+  (program cl-program))
+
+(cffi:defcfun ("clReleaseProgram" %release-program) cl-error-code
+  (program cl-program))
+
+(cffi:defcfun ("clBuildProgram" %build-program) cl-error-code
+  (program cl-program)
+  (num-devices cl-uint)
+  (device-list (:pointer cl-device-id))
+  (options :string)
+  (pfn-notify :pointer)
+  (user-data (:pointer :void)))
+
+(cffi:defcfun ("clCompileProgram" %compile-program) cl-error-code
+  (program cl-program)
+  (num-devices cl-uint)
+  (device-list (:pointer cl-device-id))
+  (options (:pointer :char))
+  (num-input-headers cl-uint)
+  (input-headers (:pointer cl-program))
+  (header-include-names (:pointer (:pointer :char)))
+  (pfn-notify :pointer)
+  (user-data (:pointer :void)))
+
+(cffi:defcfun ("clLinkProgram" %link-program) cl-program
+  (context cl-context)
+  (num-devices cl-uint)
+  (device-list (:pointer cl-device-id))
+  (options (:pointer :char))
+  (num-input-programs cl-uint)
+  (input-programs (:pointer cl-program))
+  (pfn-notify :pointer)
+  (user-data (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clSetProgramReleaseCallback" set-program-release-callback) cl-int
+  (program cl-program)
+  (pfn-notify :pointer)
+  (user-data (:pointer :void)))
+
+(cffi:defcfun ("clSetProgramSpecializationConstant" set-program-specialization-constant) cl-int
+  (program cl-program)
+  (spec-id cl-uint)
+  (spec-size :size)
+  (spec-value (:pointer :void)))
+
+(cffi:defcfun ("clUnloadPlatformCompiler" %unload-platform-compiler) cl-error-code
+  (platform cl-platform-id))
+
+(cffi:defcfun ("clGetProgramInfo" %get-program-info) cl-int
+  (program cl-program)
+  (param-name cl-program-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clGetProgramBuildInfo" %get-program-build-info) cl-int
+  (program cl-program)
+  (device cl-device-id)
+  (param-name cl-program-build-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+;;; Kernel Object APIs
+
+(cffi:defcfun ("clCreateKernel" %create-kernel) cl-kernel
+  (program cl-program)
+  (kernel-name :string)
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateKernelsInProgram" %create-kernels-in-program) cl-error-code
+  (program cl-program)
+  (num-kernels cl-uint)
+  (kernels (:pointer cl-kernel))
+  (num-kernels-ret (:pointer cl-uint)))
+
+(cffi:defcfun ("clCloneKernel" %clone-kernel) cl-kernel
+  (source-kernel cl-kernel)
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clRetainKernel" %retain-kernel) cl-error-code
+  (kernel cl-kernel))
+
+(cffi:defcfun ("clReleaseKernel" %release-kernel) cl-error-code
+  (kernel cl-kernel))
+
+(cffi:defcfun ("clSetKernelArg" %set-kernel-arg) cl-error-code
+  (kernel cl-kernel)
+  (arg-index cl-uint)
+  (arg-size :size)
+  (arg-value (:pointer :void)))
+
+(cffi:defcfun ("clSetKernelArgSVMPointer" set-kernel-arg-svm-pointer) cl-int
+  (kernel cl-kernel)
+  (arg-index cl-uint)
+  (arg-value (:pointer :void)))
+
+(cffi:defcfun ("clSetKernelExecInfo" set-kernel-exec-info) cl-int
+  (kernel cl-kernel)
+  (param-name cl-kernel-exec-info)
+  (param-value-size :size)
+  (param-value (:pointer :void)))
+
+(cffi:defcfun ("clGetKernelInfo" %get-kernel-info) cl-int
+  (kernel cl-kernel)
+  (param-name cl-kernel-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clGetKernelArgInfo" %get-kernel-arg-info) cl-int
+  (kernel cl-kernel)
+  (arg-indx cl-uint)
+  (param-name cl-kernel-arg-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clGetKernelWorkGroupInfo" %get-kernel-work-group-info) cl-int
+  (kernel cl-kernel)
+  (device cl-device-id)
+  (param-name cl-kernel-work-group-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clGetKernelSubGroupInfo" %get-kernel-sub-group-info) cl-int
+  (kernel cl-kernel)
+  (device cl-device-id)
+  (param-name cl-kernel-sub-group-info)
+  (input-value-size :size)
+  (input-value (:pointer :void))
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+;;; Event Object APIs
+
+(cffi:defcfun ("clWaitForEvents" %wait-for-events) cl-error-code
+  (num-events cl-uint)
+  (event-list (:pointer cl-event)))
+
+(cffi:defcfun ("clGetEventInfo" %get-event-info) cl-error-code
+  (event cl-event)
+  (param-name cl-event-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+(cffi:defcfun ("clCreateUserEvent" %create-user-event) cl-event
+  (context cl-context)
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clRetainEvent" %retain-event) cl-error-code
+  (event cl-event))
+
+(cffi:defcfun ("clReleaseEvent" %release-event) cl-error-code
+  (event cl-event))
+
+(cffi:defcfun ("clSetUserEventStatus" %set-user-event-status) cl-error-code
+  (event cl-event)
+  (execution-status cl-int))
+
+(cffi:defcfun ("clSetEventCallback" set-event-callback) cl-int
+  (event cl-event)
+  (command-exec-callback-type cl-int)
+  (pfn-notify :pointer)
+  (user-data (:pointer :void)))
+
+;;; Profiling APIs
+
+(cffi:defcfun ("clGetEventProfilingInfo" %get-event-profiling-info) cl-error-code
+  (event cl-event)
+  (param-name cl-profiling-info)
+  (param-value-size :size)
+  (param-value (:pointer :void))
+  (param-value-size-ret (:pointer :size)))
+
+;;; Flush and Finish APIs
+
+(cffi:defcfun ("clFlush" %flush) cl-error-code
+  (command-queue cl-command-queue))
+
+(cffi:defcfun ("clFinish" %finish) cl-error-code
+  (command-queue cl-command-queue))
+
+;;; Enqueued Commands APIs
+
+(cffi:defcfun ("clEnqueueReadBuffer" %enqueue-read-buffer) cl-error-code
+  (command-queue cl-command-queue)
+  (buffer cl-mem)
+  (blocking-read cl-bool)
+  (offset :size)
+  (size :size)
+  (ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueReadBufferRect" enqueue-read-buffer-rect) cl-int
+  (command-queue cl-command-queue)
+  (buffer cl-mem)
+  (blocking-read cl-bool)
+  (buffer-origin (:pointer :size))
+  (host-origin (:pointer :size))
+  (region (:pointer :size))
+  (buffer-row-pitch :size)
+  (buffer-slice-pitch :size)
+  (host-row-pitch :size)
+  (host-slice-pitch :size)
+  (ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueWriteBuffer" enqueue-write-buffer) cl-int
+  (command-queue cl-command-queue)
+  (buffer cl-mem)
+  (blocking-write cl-bool)
+  (offset :size)
+  (size :size)
+  (ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueWriteBufferRect" enqueue-write-buffer-rect) cl-int
+  (command-queue cl-command-queue)
+  (buffer cl-mem)
+  (blocking-write cl-bool)
+  (buffer-origin (:pointer :size))
+  (host-origin (:pointer :size))
+  (region (:pointer :size))
+  (buffer-row-pitch :size)
+  (buffer-slice-pitch :size)
+  (host-row-pitch :size)
+  (host-slice-pitch :size)
+  (ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueFillBuffer" enqueue-fill-buffer) cl-int
+  (command-queue cl-command-queue)
+  (buffer cl-mem)
+  (pattern (:pointer :void))
+  (pattern-size :size)
+  (offset :size)
+  (size :size)
+  (ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueCopyBuffer" enqueue-copy-buffer) cl-int
+  (command-queue cl-command-queue)
+  (src-buffer cl-mem)
+  (dst-buffer cl-mem)
+  (src-offset :size)
+  (dst-offset :size)
+  (size :size)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueCopyBufferRect" enqueue-copy-buffer-rect) cl-int
+  (command-queue cl-command-queue)
+  (src-buffer cl-mem)
+  (dst-buffer cl-mem)
+  (src-origin (:pointer :size))
+  (dst-origin (:pointer :size))
+  (region (:pointer :size))
+  (src-row-pitch :size)
+  (src-slice-pitch :size)
+  (dst-row-pitch :size)
+  (dst-slice-pitch :size)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueReadImage" enqueue-read-image) cl-int
+  (command-queue cl-command-queue)
+  (image cl-mem)
+  (blocking-read cl-bool)
+  (origin (:pointer :size))
+  (region (:pointer :size))
+  (row-pitch :size)
+  (slice-pitch :size)
+  (ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueWriteImage" enqueue-write-image) cl-int
+  (command-queue cl-command-queue)
+  (image cl-mem)
+  (blocking-write cl-bool)
+  (origin (:pointer :size))
+  (region (:pointer :size))
+  (input-row-pitch :size)
+  (input-slice-pitch :size)
+  (ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueFillImage" enqueue-fill-image) cl-int
+  (command-queue cl-command-queue)
+  (image cl-mem)
+  (fill-color (:pointer :void))
+  (origin (:pointer :size))
+  (region (:pointer :size))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueCopyImage" enqueue-copy-image) cl-int
+  (command-queue cl-command-queue)
+  (src-image cl-mem)
+  (dst-image cl-mem)
+  (src-origin (:pointer :size))
+  (dst-origin (:pointer :size))
+  (region (:pointer :size))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueCopyImageToBuffer" enqueue-copy-image-to-buffer) cl-int
+  (command-queue cl-command-queue)
+  (src-image cl-mem)
+  (dst-buffer cl-mem)
+  (src-origin (:pointer :size))
+  (region (:pointer :size))
+  (dst-offset :size)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueCopyBufferToImage" enqueue-copy-buffer-to-image) cl-int
+  (command-queue cl-command-queue)
+  (src-buffer cl-mem)
+  (dst-image cl-mem)
+  (src-offset :size)
+  (dst-origin (:pointer :size))
+  (region (:pointer :size))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueMapBuffer" enqueue-map-buffer) (:pointer :void)
+  (command-queue cl-command-queue)
+  (buffer cl-mem)
+  (blocking-map cl-bool)
+  (map-flags cl-map-flags)
+  (offset :size)
+  (size :size)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clEnqueueMapImage" enqueue-map-image) (:pointer :void)
+  (command-queue cl-command-queue)
+  (image cl-mem)
+  (blocking-map cl-bool)
+  (map-flags cl-map-flags)
+  (origin (:pointer :size))
+  (region (:pointer :size))
+  (image-row-pitch (:pointer :size))
+  (image-slice-pitch (:pointer :size))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clEnqueueUnmapMemObject" enqueue-unmap-mem-object) cl-int
+  (command-queue cl-command-queue)
+  (memobj cl-mem)
+  (mapped-ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueMigrateMemObjects" enqueue-migrate-mem-objects) cl-int
+  (command-queue cl-command-queue)
+  (num-mem-objects cl-uint)
+  (mem-objects (:pointer cl-mem))
+  (flags cl-mem-migration-flags)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueNDRangeKernel" %enqueue-nd-range-kernel) cl-error-code
+  (command-queue cl-command-queue)
+  (kernel cl-kernel)
+  (work-dim cl-uint)
+  (global-work-offset (:pointer :size))
+  (global-work-size (:pointer :size))
+  (local-work-size (:pointer :size))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueNativeKernel" enqueue-native-kernel) cl-int
+  (command-queue cl-command-queue)
+  (user-func :pointer)
+  (args (:pointer :void))
+  (cb-args :size)
+  (num-mem-objects cl-uint)
+  (mem-list (:pointer cl-mem))
+  (args-mem-loc (:pointer (:pointer :void)))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueMarkerWithWaitList" enqueue-marker-with-wait-list) cl-int
+  (command-queue cl-command-queue)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueBarrierWithWaitList" enqueue-barrier-with-wait-list) cl-int
+  (command-queue cl-command-queue)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueSVMFree" %enqueue-svm-free) cl-error-code
+  (command-queue cl-command-queue)
+  (num-svm-pointers cl-uint)
+  (svm-pointers (:pointer (:pointer :void)))
+  (pfn-free-func :pointer)
+  (user-data :pointer)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueSVMMemcpy" %enqueue-svm-memcpy) cl-error-code
+  (command-queue cl-command-queue)
+  (blocking-copy cl-bool)
+  (dst-ptr (:pointer :void))
+  (src-ptr (:pointer :void))
+  (size :size)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueSVMMemfill" %enqueue-svm-memfill) cl-error-code
+  (command-queue cl-command-queue)
+  (svm-ptr (:pointer :void))
+  (pattern (:pointer :void))
+  (pattern-size :size)
+  (size :size)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueSVMMap" %enqueue-svm-map) cl-error-code
+  (command-queue cl-command-queue)
+  (blocking-map cl-bool)
+  (flags cl-map-flags)
+  (svm-ptr (:pointer :void))
+  (size :size)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueSVMUnmap" %enqueue-svm-unmap) cl-error-code
+  (command-queue cl-command-queue)
+  (svm-ptr (:pointer :void))
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueSVMMigrateMem" %enqueue-svm-migrate-mem) cl-error-code
+  (command-queue cl-command-queue)
+  (num-svm-pointers cl-uint)
+  (svm-pointers (:pointer (:pointer :void)))
+  (sizes (:pointer :size))
+  (flags cl-mem-migration-flags)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
+
+;;; Extension function access
+
+(cffi:defcfun ("clGetExtensionFunctionAddressForPlatform"
+               get-extension-function-address-for-platform)
+    (:pointer :void)
+  (platform cl-platform-id)
+  (func-name :string))
+
+;;; Deprecated OpenCL 1.0 APIs
+
+(cffi:defcfun ("clSetCommandQueueProperty" set-command-queue-property) cl-int
+  (command-queue cl-command-queue)
+  (properties cl-command-queue-properties)
+  (enable cl-bool)
+  (old-properties (:pointer cl-command-queue-properties)))
+
+;;; Deprecated OpenCL 1.1 APIs
+
+(cffi:defcfun ("clCreateImage2D" create-image-2d) cl-mem
+  (context cl-context)
+  (flags cl-mem-flags)
+  (image-format (:pointer (:struct cl-image-format)))
+  (image-width :size)
+  (image-height :size)
+  (image-row-pitch :size)
+  (host-ptr (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateImage3D" create-image-3d) cl-mem
+  (context cl-context)
+  (flags cl-mem-flags)
+  (image-format (:pointer (:struct cl-image-format)))
+  (image-width :size)
+  (image-height :size)
+  (image-depth :size)
+  (image-row-pitch :size)
+  (image-slice-pitch :size)
+  (host-ptr (:pointer :void))
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clEnqueueMarker" enqueue-marker) cl-int
+  (command-queue cl-command-queue)
+  (event (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueWaitForEvents" %enqueue-wait-for-events) cl-error-code
+  (command-queue cl-command-queue)
+  (num-events cl-uint)
+  (event-list (:pointer cl-event)))
+
+(cffi:defcfun ("clEnqueueBarrier" enqueue-barrier) cl-int
+  (command-queue cl-command-queue))
+
+(cffi:defcfun ("clUnloadCompiler" unload-compiler) cl-int)
+
+(cffi:defcfun ("clGetExtensionFunctionAddress" get-extension-function-address) (:pointer :void)
+  (func-name :string))
+
+;;; Deprecated OpenCL 2.0 APIs
+
+(cffi:defcfun ("clCreateCommandQueue" %create-command-queue) cl-command-queue
+  (context cl-context)
+  (device cl-device-id)
+  (properties cl-command-queue-properties)
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clCreateSampler" create-sampler) cl-sampler
+  (context cl-context)
+  (normalized-coords cl-bool)
+  (addressing-mode cl-addressing-mode)
+  (filter-mode cl-filter-mode)
+  (errcode-ret (:pointer cl-int)))
+
+(cffi:defcfun ("clEnqueueTask" enqueue-task) cl-int
+  (command-queue cl-command-queue)
+  (kernel cl-kernel)
+  (num-events-in-wait-list cl-uint)
+  (event-wait-list (:pointer cl-event))
+  (event (:pointer cl-event)))
diff --git a/src/command-queue.lisp b/src/command-queue.lisp
new file mode 100644
index 0000000..ec9f89c
--- /dev/null
+++ b/src/command-queue.lisp
@@ -0,0 +1,38 @@
+(in-package #:ocl)
+
+(defun create-command-queue-with-properties (context device &key queue-properties queue-size)
+  (let ((properties '(0)))
+    (when queue-properties
+      (push (cffi:foreign-bitfield-value 'cl-command-queue-properties queue-properties) properties)
+      (push :queue-properties properties))
+    (when queue-size
+      (push queue-size properties)
+      (push :queue-size properties))
+    (with-foreign-sequence (c-properties properties 'cl-queue-properties)
+      (check-error-arg (%create-command-queue-with-properties context device c-properties)))))
+
+(defun retain-command-queue (command-queue)
+  (check-error (%retain-command-queue command-queue)))
+
+(defun release-command-queue (command-queue)
+  (check-error (%release-command-queue command-queue)))
+
+(defparameter +command-queue-info-type-alist+
+  '((:queue-context          . cl-context)
+    (:queue-device           . cl-device-id)
+    (:queue-reference-count  . cl-uint)
+    (:queue-properties       . cl-command-queue-properties)
+    (:queue-properties-array . (:pointer cl-queue-properties))
+    (:queue-size             . cl-uint)
+    (:queue-device-default   . cl-command-queue)))
+
+(wrap-get-info-function get-command-queue-info %get-command-queue-info
+                        +command-queue-info-type-alist+)
+
+(defmacro with-command-queue ((queue context device &key queue-properties queue-size) &body body)
+  `(let ((,queue (create-command-queue-with-properties ,context ,device
+                                                       :queue-properties ,queue-properties
+                                                       :queue-size ,queue-size)))
+     (unwind-protect
+          (progn ,@body)
+       (release-command-queue ,queue))))
diff --git a/src/constants.lisp b/src/constants.lisp
new file mode 100644
index 0000000..58da3f2
--- /dev/null
+++ b/src/constants.lisp
@@ -0,0 +1,558 @@
+(in-package #:ocl)
+
+;;; Error Codes
+;; (defconstant +success+                                  0)
+;; (defconstant +device-not-found+                         -1)
+;; (defconstant +device-not-available+                     -2)
+;; (defconstant +compiler-not-available+                   -3)
+;; (defconstant +mem-object-allocation-failure+            -4)
+;; (defconstant +out-of-resources+                         -5)
+;; (defconstant +out-of-host-memory+                       -6)
+;; (defconstant +profiling-info-not-available+             -7)
+;; (defconstant +mem-copy-overlap+                         -8)
+;; (defconstant +image-format-mismatch+                    -9)
+;; (defconstant +image-format-not-supported+               -10)
+;; (defconstant +build-program-failure+                    -11)
+;; (defconstant +map-failure+                              -12)
+;; (defconstant +misaligned-sub-buffer-offset+             -13)
+;; (defconstant +exec-status-error-for-events-in-wait-list+ -14)
+;; (defconstant +compile-program-failure+                  -15)
+;; (defconstant +linker-not-available+                     -16)
+;; (defconstant +link-program-failure+                     -17)
+;; (defconstant +device-partition-failed+                  -18)
+;; (defconstant +kernel-arg-info-not-available+            -19)
+;; (defconstant +invalid-value+                            -30)
+;; (defconstant +invalid-device-type+                      -31)
+;; (defconstant +invalid-platform+                         -32)
+;; (defconstant +invalid-device+                           -33)
+;; (defconstant +invalid-context+                          -34)
+;; (defconstant +invalid-queue-properties+                 -35)
+;; (defconstant +invalid-command-queue+                    -36)
+;; (defconstant +invalid-host-ptr+                         -37)
+;; (defconstant +invalid-mem-object+                       -38)
+;; (defconstant +invalid-image-format-descriptor+          -39)
+;; (defconstant +invalid-image-size+                       -40)
+;; (defconstant +invalid-sampler+                          -41)
+;; (defconstant +invalid-binary+                           -42)
+;; (defconstant +invalid-build-options+                    -43)
+;; (defconstant +invalid-program+                          -44)
+;; (defconstant +invalid-program-executable+               -45)
+;; (defconstant +invalid-kernel-name+                      -46)
+;; (defconstant +invalid-kernel-definition+                -47)
+;; (defconstant +invalid-kernel+                           -48)
+;; (defconstant +invalid-arg-index+                        -49)
+;; (defconstant +invalid-arg-value+                        -50)
+;; (defconstant +invalid-arg-size+                         -51)
+;; (defconstant +invalid-kernel-args+                      -52)
+;; (defconstant +invalid-work-dimension+                   -53)
+;; (defconstant +invalid-work-group-size+                  -54)
+;; (defconstant +invalid-work-item-size+                   -55)
+;; (defconstant +invalid-global-offset+                    -56)
+;; (defconstant +invalid-event-wait-list+                  -57)
+;; (defconstant +invalid-event+                            -58)
+;; (defconstant +invalid-operation+                        -59)
+;; (defconstant +invalid-gl-object+                        -60)
+;; (defconstant +invalid-buffer-size+                      -61)
+;; (defconstant +invalid-mip-level+                        -62)
+;; (defconstant +invalid-global-work-size+                 -63)
+;; (defconstant +invalid-property+                         -64)
+;; (defconstant +invalid-image-descriptor+                 -65)
+;; (defconstant +invalid-compiler-options+                 -66)
+;; (defconstant +invalid-linker-options+                   -67)
+;; (defconstant +invalid-device-partition-count+           -68)
+;; (defconstant +invalid-pipe-size+                        -69)
+;; (defconstant +invalid-device-queue+                     -70)
+;; (defconstant +invalid-spec-id+                          -71)
+;; (defconstant +max-size-restriction-exceeded+            -72)
+
+;;; cl-bool
+;; (defconstant +false+ 0)
+;; (defconstant +true+ 1)
+;; (defconstant +blocking+ +true+)
+;; (defconstant +non-blocking+ +false+)
+
+
+;;; cl-platform-info
+;; (defconstant +platform-profile+ #x0900)
+;; (defconstant +platform-version+ #x0901)
+;; (defconstant +platform-name+ #x0902)
+;; (defconstant +platform-vendor+ #x0903)
+;; (defconstant +platform-extensions+ #x0904)
+;; (defconstant +platform-host-timer-resolution+ #x0905)
+;; (defconstant +platform-numeric-version+ #x0906)
+;; (defconstant +platform-extensions-with-version+ #x0907)
+
+;;; cl-device-type - bitfield
+;; (defconstant +device-type-default+ #x1)
+;; (defconstant +device-type-cpu+ #x2)
+;; (defconstant +device-type-gpu+ #x4)
+;; (defconstant +device-type-accelerator+ #x8)
+;; (defconstant +device-type-custom+ #x10)
+;; (defconstant +device-type-all+ #xffffffff)
+
+;;; cl-device-info
+;; (defconstant +device-type+ #x1000)
+;; (defconstant +device-vendor-id+ #x1001)
+;; (defconstant +device-max-compute-units+ #x1002)
+;; (defconstant +device-max-work-item-dimensions+ #x1003)
+;; (defconstant +device-max-work-group-size+ #x1004)
+;; (defconstant +device-max-work-item-sizes+ #x1005)
+;; (defconstant +device-preferred-vector-width-char+ #x1006)
+;; (defconstant +device-preferred-vector-width-short+ #x1007)
+;; (defconstant +device-preferred-vector-width-int+ #x1008)
+;; (defconstant +device-preferred-vector-width-long+ #x1009)
+;; (defconstant +device-preferred-vector-width-float+ #x100a)
+;; (defconstant +device-preferred-vector-width-double+ #x100b)
+;; (defconstant +device-max-clock-frequency+ #x100c)
+;; (defconstant +device-address-bits+ #x100d)
+;; (defconstant +device-max-read-image-args+ #x100e)
+;; (defconstant +device-max-write-image-args+ #x100f)
+;; (defconstant +device-max-mem-alloc-size+ #x1010)
+;; (defconstant +device-image2d-max-width+ #x1011)
+;; (defconstant +device-image2d-max-height+ #x1012)
+;; (defconstant +device-image3d-max-width+ #x1013)
+;; (defconstant +device-image3d-max-height+ #x1014)
+;; (defconstant +device-image3d-max-depth+ #x1015)
+;; (defconstant +device-image-support+ #x1016)
+;; (defconstant +device-max-parameter-size+ #x1017)
+;; (defconstant +device-max-samplers+ #x1018)
+;; (defconstant +device-mem-base-addr-align+ #x1019)
+;; (defconstant +device-min-data-type-align-size+ #x101a)
+;; (defconstant +device-single-fp-config+ #x101b)
+;; (defconstant +device-global-mem-cache-type+ #x101c)
+;; (defconstant +device-global-mem-cacheline-size+ #x101d)
+;; (defconstant +device-global-mem-cache-size+ #x101e)
+;; (defconstant +device-global-mem-size+ #x101f)
+;; (defconstant +device-max-constant-buffer-size+ #x1020)
+;; (defconstant +device-max-constant-args+ #x1021)
+;; (defconstant +device-local-mem-type+ #x1022)
+;; (defconstant +device-local-mem-size+ #x1023)
+;; (defconstant +device-error-correction-support+ #x1024)
+;; (defconstant +device-profiling-timer-resolution+ #x1025)
+;; (defconstant +device-endian-little+ #x1026)
+;; (defconstant +device-available+ #x1027)
+;; (defconstant +device-compiler-available+ #x1028)
+;; (defconstant +device-execution-capabilities+ #x1029)
+;; (defconstant +device-queue-properties+ #x102a)
+;; (defconstant +device-queue-on-host-properties+ #x102a)
+;; (defconstant +device-name+ #x102b)
+;; (defconstant +device-vendor+ #x102c)
+;; (defconstant +driver-version+ #x102d)
+;; (defconstant +device-profile+ #x102e)
+;; (defconstant +device-version+ #x102f)
+;; (defconstant +device-extensions+ #x1030)
+;; (defconstant +device-platform+ #x1031)
+;; (defconstant +device-double-fp-config+ #x1032)
+;; (defconstant +device-preferred-vector-width-half+ #x1034)
+;; (defconstant +device-host-unified-memory+ #x1035)
+;; (defconstant +device-native-vector-width-char+ #x1036)
+;; (defconstant +device-native-vector-width-short+ #x1037)
+;; (defconstant +device-native-vector-width-int+ #x1038)
+;; (defconstant +device-native-vector-width-long+ #x1039)
+;; (defconstant +device-native-vector-width-float+ #x103a)
+;; (defconstant +device-native-vector-width-double+ #x103b)
+;; (defconstant +device-native-vector-width-half+ #x103c)
+;; (defconstant +device-opencl-c-version+ #x103d)
+;; (defconstant +device-linker-available+ #x103e)
+;; (defconstant +device-built-in-kernels+ #x103f)
+;; (defconstant +device-image-max-buffer-size+ #x1040)
+;; (defconstant +device-image-max-array-size+ #x1041)
+;; (defconstant +device-parent-device+ #x1042)
+;; (defconstant +device-partition-max-sub-devices+ #x1043)
+;; (defconstant +device-partition-properties+ #x1044)
+;; (defconstant +device-partition-affinity-domain+ #x1045)
+;; (defconstant +device-partition-type+ #x1046)
+;; (defconstant +device-reference-count+ #x1047)
+;; (defconstant +device-preferred-interop-user-sync+ #x1048)
+;; (defconstant +device-printf-buffer-size+ #x1049)
+;; (defconstant +device-image-pitch-alignment+ #x104a)
+;; (defconstant +device-image-base-address-alignment+ #x104b)
+;; (defconstant +device-max-read-write-image-args+ #x104c)
+;; (defconstant +device-max-global-variable-size+ #x104d)
+;; (defconstant +device-queue-on-device-properties+ #x104e)
+;; (defconstant +device-queue-on-device-preferred-size+ #x104f)
+;; (defconstant +device-queue-on-device-max-size+ #x1050)
+;; (defconstant +device-max-on-device-queues+ #x1051)
+;; (defconstant +device-max-on-device-events+ #x1052)
+;; (defconstant +device-svm-capabilities+ #x1053)
+;; (defconstant +device-global-variable-preferred-total-size+ #x1054)
+;; (defconstant +device-max-pipe-args+ #x1055)
+;; (defconstant +device-pipe-max-active-reservations+ #x1056)
+;; (defconstant +device-pipe-max-packet-size+ #x1057)
+;; (defconstant +device-preferred-platform-atomic-alignment+ #x1058)
+;; (defconstant +device-preferred-global-atomic-alignment+ #x1059)
+;; (defconstant +device-preferred-local-atomic-alignment+ #x105a)
+;; (defconstant +device-il-version+ #x105b)
+;; (defconstant +device-max-num-sub-groups+ #x105c)
+;; (defconstant +device-sub-group-independent-forward-progress+ #x105d)
+;; (defconstant +device-numeric-version+ #x105e)
+;; (defconstant +device-extensions-with-version+ #x1060)
+;; (defconstant +device-ils-with-version+ #x1061)
+;; (defconstant +device-built-in-kernels-with-version+ #x1062)
+;; (defconstant +device-atomic-memory-capabilities+ #x1063)
+;; (defconstant +device-atomic-fence-capabilities+ #x1064)
+;; (defconstant +device-non-uniform-work-group-support+ #x1065)
+;; (defconstant +device-opencl-c-all-versions+ #x1066)
+;; (defconstant +device-preferred-work-group-size-multiple+ #x1067)
+;; (defconstant +device-work-group-collective-functions-support+ #x1068)
+;; (defconstant +device-generic-address-space-support+ #x1069)
+;; (defconstant +device-opencl-c-features+ #x106f)
+;; (defconstant +device-device-enqueue-capabilities+ #x1070)
+;; (defconstant +device-pipe-support+ #x1071)
+;; (defconstant +device-latest-conformance-version-passed+ #x1072)
+
+;;; cl-device-fp-config - bitfield
+;; (defconstant +fp-denorm+ #x1)
+;; (defconstant +fp-inf-nan+ #x2)
+;; (defconstant +fp-round-to-nearest+ #x4)
+;; (defconstant +fp-round-to-zero+ #x8)
+;; (defconstant +fp-round-to-inf+ #x10)
+;; (defconstant +fp-fma+ #x20)
+;; (defconstant +fp-soft-float+ #x40)
+;; (defconstant +fp-correctly-rounded-divide-sqrt+ #x80)
+
+;;; cl-device-mem-cache-type
+;; (defconstant +none+ #x0)
+;; (defconstant +read-only-cache+ #x1)
+;; (defconstant +read-write-cache+ #x2)
+
+;;; cl-device-local-mem-type
+;; (defconstant +local+ #x1)
+;; (defconstant +global+ #x2)
+
+;;; cl-device-exec-capabilities - bitfield
+;; (defconstant +exec-kernel+ #x1)
+;; (defconstant +exec-native-kernel+ #x2)
+
+;;; cl-command-queue-properties - bitfield
+;; (defconstant +queue-out-of-order-exec-mode-enable+ #x1)
+;; (defconstant +queue-profiling-enable+ #x2)
+;; (defconstant +queue-on-device+ #x4)
+;; (defconstant +queue-on-device-default+ #x8)
+
+;;; cl-context-info
+;; (defconstant +context-reference-count+ #x1080)
+;; (defconstant +context-devices+ #x1081)
+;; (defconstant +context-properties+ #x1082)
+;; (defconstant +context-num-devices+ #x1083)
+
+;;; cl-context-properties
+;; (defconstant +context-platform+ #x1084)
+;; (defconstant +context-interop-user-sync+ #x1085)
+
+;;; cl-device-partition-property
+(defconstant +device-partition-equally+ #x1086)
+(defconstant +device-partition-by-counts+ #x1087)
+(defconstant +device-partition-by-counts-list-end+ #x0)
+(defconstant +device-partition-by-affinity-domain+ #x1088)
+
+
+;;; cl-device-affinity-domain
+;; (defconstant +device-affinity-domain-numa+ #x1)
+;; (defconstant +device-affinity-domain-l4-cache+ #x2)
+;; (defconstant +device-affinity-domain-l3-cache+ #x4)
+;; (defconstant +device-affinity-domain-l2-cache+ #x8)
+;; (defconstant +device-affinity-domain-l1-cache+ #x10)
+;; (defconstant +device-affinity-domain-next-partitionable+ #x20)
+
+;;; cl-device-svm-capabilities
+;; (defconstant +device-svm-coarse-grain-buffer+ #x1)
+;; (defconstant +device-svm-fine-grain-buffer+ #x2)
+;; (defconstant +device-svm-fine-grain-system+ #x4)
+;; (defconstant +device-svm-atomics+ #x8)
+
+;;; cl-command-queue-info
+;; (defconstant +queue-context+ #x1090)
+;; (defconstant +queue-device+ #x1091)
+;; (defconstant +queue-reference-count+ #x1092)
+;; (defconstant +queue-properties+ #x1093)
+;; (defconstant +queue-size+ #x1094)
+;; (defconstant +queue-device-default+ #x1095)
+;; (defconstant +queue-properties-array+ #x1098)
+
+;;; cl-mem-flags and cl-svm-mem-flags - bitfield
+(defconstant +mem-read-write+ #x1)
+(defconstant +mem-write-only+ #x2)
+(defconstant +mem-read-only+ #x4)
+(defconstant +mem-use-host-ptr+ #x8)
+(defconstant +mem-alloc-host-ptr+ #x10)
+(defconstant +mem-copy-host-ptr+ #x20)
+(defconstant +mem-host-write-only+ #x80)
+(defconstant +mem-host-read-only+ #x100)
+(defconstant +mem-host-no-access+ #x200)
+(defconstant +mem-svm-fine-grain-buffer+ #x400)
+(defconstant +mem-svm-atomics+ #x800)
+(defconstant +mem-kernel-read-and-write+ #x1000)
+
+
+;;; cl-mem-migration-flags - bitfield
+;; (defconstant +migrate-mem-object-host+ #x1)
+;; (defconstant +migrate-mem-object-content-undefined+ #x2)
+
+;;; cl-channel-order
+;; (defconstant +r+ #x10b0)
+;; (defconstant +a+ #x10b1)
+;; (defconstant +rg+ #x10b2)
+;; (defconstant +ra+ #x10b3)
+;; (defconstant +rgb+ #x10b4)
+;; (defconstant +rgba+ #x10b5)
+;; (defconstant +bgra+ #x10b6)
+;; (defconstant +argb+ #x10b7)
+;; (defconstant +intensity+ #x10b8)
+;; (defconstant +luminance+ #x10b9)
+;; (defconstant +rx+ #x10ba)
+;; (defconstant +rgx+ #x10bb)
+;; (defconstant +rgbx+ #x10bc)
+;; (defconstant +depth+ #x10bd)
+;; (defconstant +depth-stencil+ #x10be)
+;; (defconstant +srgb+ #x10bf)
+;; (defconstant +srgbx+ #x10c0)
+;; (defconstant +srgba+ #x10c1)
+;; (defconstant +sbgra+ #x10c2)
+;; (defconstant +abgr+ #x10c3)
+
+;;; cl-channel-type
+;; (defconstant +snorm-int8+ #x10d0)
+;; (defconstant +snorm-int16+ #x10d1)
+;; (defconstant +unorm-int8+ #x10d2)
+;; (defconstant +unorm-int16+ #x10d3)
+;; (defconstant +unorm-short-565+ #x10d4)
+;; (defconstant +unorm-short-555+ #x10d5)
+;; (defconstant +unorm-int-101010+ #x10d6)
+;; (defconstant +signed-int8+ #x10d7)
+;; (defconstant +signed-int16+ #x10d8)
+;; (defconstant +signed-int32+ #x10d9)
+;; (defconstant +unsigned-int8+ #x10da)
+;; (defconstant +unsigned-int16+ #x10db)
+;; (defconstant +unsigned-int32+ #x10dc)
+;; (defconstant +half-float+ #x10dd)
+;; (defconstant +float+ #x10de)
+;; (defconstant +unorm-int24+ #x10df)
+;; (defconstant +unorm-int-101010-2+ #x10e0)
+
+;;; cl-mem-object-type
+;; (defconstant +mem-object-buffer+ #x10f0)
+;; (defconstant +mem-object-image2d+ #x10f1)
+;; (defconstant +mem-object-image3d+ #x10f2)
+;; (defconstant +mem-object-image2d-array+ #x10f3)
+;; (defconstant +mem-object-image1d+ #x10f4)
+;; (defconstant +mem-object-image1d-array+ #x10f5)
+;; (defconstant +mem-object-image1d-buffer+ #x10f6)
+;; (defconstant +mem-object-pipe+ #x10f7)
+
+;;; cl-mem-info
+;; (defconstant +mem-type+ #x1100)
+;; (defconstant +mem-flags+ #x1101)
+;; (defconstant +mem-size+ #x1102)
+;; (defconstant +mem-host-ptr+ #x1103)
+;; (defconstant +mem-map-count+ #x1104)
+;; (defconstant +mem-reference-count+ #x1105)
+;; (defconstant +mem-context+ #x1106)
+;; (defconstant +mem-associated-memobject+ #x1107)
+;; (defconstant +mem-offset+ #x1108)
+;; (defconstant +mem-uses-svm-pointer+ #x1109)
+;; (defconstant +mem-properties+ #x110a)
+
+;;; cl-image-info
+;; (defconstant +image-format+ #x1110)
+;; (defconstant +image-element-size+ #x1111)
+;; (defconstant +image-row-pitch+ #x1112)
+;; (defconstant +image-slice-pitch+ #x1113)
+;; (defconstant +image-width+ #x1114)
+;; (defconstant +image-height+ #x1115)
+;; (defconstant +image-depth+ #x1116)
+;; (defconstant +image-array-size+ #x1117)
+;; (defconstant +image-buffer+ #x1118)
+;; (defconstant +image-num-mip-levels+ #x1119)
+;; (defconstant +image-num-samples+ #x111a)
+
+;;; cl-pipe-info
+;; (defconstant +pipe-packet-size+ #x1120)
+;; (defconstant +pipe-max-packets+ #x1121)
+;; (defconstant +pipe-properties+ #x1122)
+
+;;; cl-addressing-mode
+;; (defconstant +address-none+ #x1130)
+;; (defconstant +address-clamp-to-edge+ #x1131)
+;; (defconstant +address-clamp+ #x1132)
+;; (defconstant +address-repeat+ #x1133)
+;; (defconstant +address-mirrored-repeat+ #x1134)
+
+;;; cl-filter-mode
+;; (defconstant +filter-nearest+ #x1140)
+;; (defconstant +filter-linear+ #x1141)
+
+;;; cl-sampler-info
+;; (defconstant +sampler-reference-count+ #x1150)
+;; (defconstant +sampler-context+ #x1151)
+;; (defconstant +sampler-normalized-coords+ #x1152)
+;; (defconstant +sampler-addressing-mode+ #x1153)
+;; (defconstant +sampler-filter-mode+ #x1154)
+;; (defconstant +sampler-mip-filter-mode+ #x1155)
+;; (defconstant +sampler-lod-min+ #x1156)
+;; (defconstant +sampler-lod-max+ #x1157)
+;; (defconstant +sampler-properties+ #x1158)
+
+
+;;; cl-map-flags - bitfield
+;; (defconstant +map-read+ #x1)
+;; (defconstant +map-write+ #x2)
+;; (defconstant +map-write-invalidate-region+ #x4)
+
+;;; cl-program-info
+;; (defconstant +program-reference-count+ #x1160)
+;; (defconstant +program-context+ #x1161)
+;; (defconstant +program-num-devices+ #x1162)
+;; (defconstant +program-devices+ #x1163)
+;; (defconstant +program-source+ #x1164)
+;; (defconstant +program-binary-sizes+ #x1165)
+;; (defconstant +program-binaries+ #x1166)
+;; (defconstant +program-num-kernels+ #x1167)
+;; (defconstant +program-kernel-names+ #x1168)
+;; (defconstant +program-il+ #x1169)
+;; (defconstant +program-scope-global-ctors-present+ #x116a)
+;; (defconstant +program-scope-global-dtors-present+ #x116b)
+
+;;; cl-program-build-info
+;; (defconstant +program-build-status+ #x1181)
+;; (defconstant +program-build-options+ #x1182)
+;; (defconstant +program-build-log+ #x1183)
+;; (defconstant +program-binary-type+ #x1184)
+;; (defconstant +program-build-global-variable-total-size+ #x1185)
+
+;;; cl-program-binary-type
+;; (defconstant +program-binary-type-none+ #x0)
+;; (defconstant +program-binary-type-compiled-object+ #x1)
+;; (defconstant +program-binary-type-library+ #x2)
+;; (defconstant +program-binary-type-executable+ #x4)
+
+;;; cl-build-status
+;; (defconstant +build-success+ 0)
+;; (defconstant +build-none+ -1)
+;; (defconstant +build-error+ -2)
+;; (defconstant +build-in-progress+ -3)
+
+;; cl-kernel-info
+;; (defconstant +kernel-function-name+ #x1190)
+;; (defconstant +kernel-num-args+ #x1191)
+;; (defconstant +kernel-reference-count+ #x1192)
+;; (defconstant +kernel-context+ #x1193)
+;; (defconstant +kernel-program+ #x1194)
+;; (defconstant +kernel-attributes+ #x1195)
+
+;;; cl-kernel-arg-info
+;; (defconstant +kernel-arg-address-qualifier+ #x1196)
+;; (defconstant +kernel-arg-access-qualifier+ #x1197)
+;; (defconstant +kernel-arg-type-name+ #x1198)
+;; (defconstant +kernel-arg-type-qualifier+ #x1199)
+;; (defconstant +kernel-arg-name+ #x119a)
+
+;;; cl-kernel-arg-address-qualifier
+;; (defconstant +kernel-arg-address-global+ #x119b)
+;; (defconstant +kernel-arg-address-local+ #x119c)
+;; (defconstant +kernel-arg-address-constant+ #x119d)
+;; (defconstant +kernel-arg-address-private+ #x119e)
+
+;;; cl-kernel-arg-access-qualifier
+;; (defconstant +kernel-arg-access-read-only+ #x11a0)
+;; (defconstant +kernel-arg-access-write-only+ #x11a1)
+;; (defconstant +kernel-arg-access-read-write+ #x11a2)
+;; (defconstant +kernel-arg-access-none+ #x11a3)
+
+;;; cl-kernel-arg-type-qualifier
+;; (defconstant +kernel-arg-type-none+ #x0)
+;; (defconstant +kernel-arg-type-const+ #x1)
+;; (defconstant +kernel-arg-type-restrict+ #x2)
+;; (defconstant +kernel-arg-type-volatile+ #x4)
+;; (defconstant +kernel-arg-type-pipe+ #x8)
+
+;;; cl-kernel-work-group-info
+;; (defconstant +kernel-work-group-size+ #x11b0)
+;; (defconstant +kernel-compile-work-group-size+ #x11b1)
+;; (defconstant +kernel-local-mem-size+ #x11b2)
+;; (defconstant +kernel-preferred-work-group-size-multiple+ #x11b3)
+;; (defconstant +kernel-private-mem-size+ #x11b4)
+;; (defconstant +kernel-global-work-size+ #x11b5)
+
+;;; cl-kernel-sub-group-info
+;; (defconstant +kernel-max-sub-group-size-for-ndrange+ #x2033)
+;; (defconstant +kernel-sub-group-count-for-ndrange+ #x2034)
+;; (defconstant +kernel-local-size-for-sub-group-count+ #x11b8)
+;; (defconstant +kernel-max-num-sub-groups+ #x11b9)
+;; (defconstant +kernel-compile-num-sub-groups+ #x11ba)
+
+;;; cl-kernel-exec-info
+;; (defconstant +kernel-exec-info-svm-ptrs+ #x11b6)
+;; (defconstant +kernel-exec-info-svm-fine-grain-system+ #x11b7)
+
+;;; cl-event-info
+;; (defconstant +event-command-queue+ #x11d0)
+;; (defconstant +event-command-type+ #x11d1)
+;; (defconstant +event-reference-count+ #x11d2)
+;; (defconstant +event-command-execution-status+ #x11d3)
+;; (defconstant +event-context+ #x11d4)
+
+;;; cl-command-type
+;; (defconstant +command-ndrange-kernel+ #x11f0)
+;; (defconstant +command-task+ #x11f1)
+;; (defconstant +command-native-kernel+ #x11f2)
+;; (defconstant +command-read-buffer+ #x11f3)
+;; (defconstant +command-write-buffer+ #x11f4)
+;; (defconstant +command-copy-buffer+ #x11f5)
+;; (defconstant +command-read-image+ #x11f6)
+;; (defconstant +command-write-image+ #x11f7)
+;; (defconstant +command-copy-image+ #x11f8)
+;; (defconstant +command-copy-image-to-buffer+ #x11f9)
+;; (defconstant +command-copy-buffer-to-image+ #x11fa)
+;; (defconstant +command-map-buffer+ #x11fb)
+;; (defconstant +command-map-image+ #x11fc)
+;; (defconstant +command-unmap-mem-object+ #x11fd)
+;; (defconstant +command-marker+ #x11fe)
+;; (defconstant +command-acquire-gl-objects+ #x11ff)
+;; (defconstant +command-release-gl-objects+ #x1200)
+;; (defconstant +command-read-buffer-rect+ #x1201)
+;; (defconstant +command-write-buffer-rect+ #x1202)
+;; (defconstant +command-copy-buffer-rect+ #x1203)
+;; (defconstant +command-user+ #x1204)
+;; (defconstant +command-barrier+ #x1205)
+;; (defconstant +command-migrate-mem-objects+ #x1206)
+;; (defconstant +command-fill-buffer+ #x1207)
+;; (defconstant +command-fill-image+ #x1208)
+;; (defconstant +command-svm-free+ #x1209)
+;; (defconstant +command-svm-memcpy+ #x120a)
+;; (defconstant +command-svm-memfill+ #x120b)
+;; (defconstant +command-svm-map+ #x120c)
+;; (defconstant +command-svm-unmap+ #x120d)
+;; (defconstant +command-svm-migrate-mem+ #x120e)
+
+;;; command execution status
+;; (defconstant +complete+ #x0)
+;; (defconstant +running+ #x1)
+;; (defconstant +submitted+ #x2)
+;; (defconstant +queued+ #x3)
+
+;;; cl-buffer-create-type
+;;(defconstant +buffer-create-type-region+ #x1220)
+
+;;; cl-profiling-info
+;; (defconstant +profiling-command-queued+ #x1280)
+;; (defconstant +profiling-command-submit+ #x1281)
+;; (defconstant +profiling-command-start+ #x1282)
+;; (defconstant +profiling-command-end+ #x1283)
+;; (defconstant +profiling-command-complete+ #x1284)
+
+;;; cl-device-atomic-capabilities - bitfield
+;; (defconstant +device-atomic-order-relaxed+ #x01)
+;; (defconstant +device-atomic-order-acq-rel+ #x02)
+;; (defconstant +device-atomic-order-seq-cst+ #x04)
+;; (defconstant +device-atomic-scope-work-item+ #x08)
+;; (defconstant +device-atomic-scope-work-group+ #x10)
+;; (defconstant +device-atomic-scope-device+ #x20)
+;; (defconstant +device-atomic-scope-all-devices+ #x40)
+
+;;; cl-device-device-enqueue-capabilities - bitfield
+;; (defconstant +device-queue-supported+ #x1)
+;; (defconstant +device-queue-replaceable-default+ #x2)
+
+;;; cl-khronos-vendor-id
+;; (defconstant +khronos-vendor-id-codeplay+ #x10004)
diff --git a/src/context.lisp b/src/context.lisp
new file mode 100644
index 0000000..45dc9b3
--- /dev/null
+++ b/src/context.lisp
@@ -0,0 +1,49 @@
+(in-package #:ocl)
+
+(defun create-context (devices &key platform iterop-user-sync-p)
+  (let ((properties '(0)))
+    (when iterop-user-sync-p
+      (push 1 properties)
+      (push :context-interop-user-sync properties))
+    (when platform
+      (push (cffi:pointer-address platform) properties)
+      (push :context-platform properties))
+    (with-foreign-sequences ((c-properties properties 'cl-context-properties)
+                             (c-devices devices 'cl-device-id num-devices))
+      (check-error-arg
+       (%create-context c-properties num-devices c-devices (cffi:null-pointer)
+                        (cffi:null-pointer))))))
+
+(defun create-context-from-type (device-type &key platform iterop-user-sync-p
+                                               (pfn-notify (cffi:null-pointer))
+                                               (user-data (cffi:null-pointer)))
+  (let ((properties '(0)))
+    (when iterop-user-sync-p
+      (push 1 properties)
+      (push :context-interop-user-sync properties))
+    (when platform
+      (push (cffi:pointer-address platform) properties)
+      (push :context-platform properties))
+    (with-foreign-sequences ((c-properties properties 'cl-context-properties))
+      (check-error-arg
+       (%create-context-from-type c-properties device-type pfn-notify user-data)))))
+
+(defun retain-context (context)
+  (check-error (%retain-context context)))
+
+(defun release-context (context)
+  (check-error (%release-context context)))
+
+(defparameter +context-info-type-alist+
+  '((:context-reference-count . cl-uint)
+    (:context-num-devices     . cl-uint)
+    (:context-devices         . (:pointer cl-device-id))
+    (:context-properties      . (:pointer cl-context-properties))))
+
+(wrap-get-info-function get-context-info %get-context-info +context-info-type-alist+)
+
+(defmacro with-context ((context devices &rest options) &body body)
+  `(let ((,context (create-context ,devices ,@options)))
+     (unwind-protect
+          (progn ,@body)
+       (release-context ,context))))
diff --git a/src/deprecated.lisp b/src/deprecated.lisp
new file mode 100644
index 0000000..ea835fe
--- /dev/null
+++ b/src/deprecated.lisp
@@ -0,0 +1,4 @@
+(in-package #:ocl)
+
+(defun create-command-queue (context device properties)
+  (check-error-arg  (%create-command-queue context device properties)))
diff --git a/src/device.lisp b/src/device.lisp
new file mode 100644
index 0000000..830ee82
--- /dev/null
+++ b/src/device.lisp
@@ -0,0 +1,176 @@
+(in-package #:ocl)
+
+(defun get-device-ids (platform device-type)
+  (let (num-devices)
+    (cffi:with-foreign-object (c-num-devices 'cl-uint)
+      (check-error (%get-device-ids platform device-type 0 (cffi:null-pointer) c-num-devices))
+      (setf num-devices (cffi:mem-ref c-num-devices 'cl-uint)))
+    (cffi:with-foreign-object (c-devices 'cl-device-id num-devices)
+      (check-error (%get-device-ids platform device-type num-devices c-devices (cffi:null-pointer)))
+      (loop :for i :below num-devices
+            :collect (cffi:mem-aref c-devices 'cl-device-id i)))))
+
+(defparameter +device-info-type-alist+
+  '((:device-type                                    . cl-device-type)
+    (:device-vendor-id                               . cl-uint)
+    (:device-max-compute-units                       . cl-uint)
+    (:device-max-work-item-dimensions                . cl-uint)
+    (:device-max-work-group-size                     . :size)
+    (:device-max-work-item-sizes                     . (:pointer :size))
+    (:device-preferred-vector-width-char             . cl-uint)
+    (:device-preferred-vector-width-short            . cl-uint)
+    (:device-preferred-vector-width-int              . cl-uint)
+    (:device-preferred-vector-width-long             . cl-uint)
+    (:device-preferred-vector-width-float            . cl-uint)
+    (:device-preferred-vector-width-double           . cl-uint)
+    (:device-max-clock-frequency                     . cl-uint)
+    (:device-address-bits                            . cl-uint)
+    (:device-max-read-image-args                     . cl-uint)
+    (:device-max-write-image-args                    . cl-uint)
+    (:device-max-mem-alloc-size                      . cl-ulong)
+    (:device-image2d-max-width                       . :size)
+    (:device-image2d-max-height                      . :size)
+    (:device-image3d-max-width                       . :size)
+    (:device-image3d-max-height                      . :size)
+    (:device-image3d-max-depth                       . :size)
+    (:device-image-support                           . cl-bool)
+    (:device-max-parameter-size                      . :size)
+    (:device-max-samplers                            . cl-uint)
+    (:device-mem-base-addr-align                     . cl-uint)
+    (:device-min-data-type-align-size                . cl-uint)
+    (:device-single-fp-config                        . cl-device-fp-config)
+    (:device-global-mem-cache-type                   . cl-device-mem-cache-type)
+    (:device-global-mem-cacheline-size               . cl-uint)
+    (:device-global-mem-cache-size                   . cl-ulong)
+    (:device-global-mem-size                         . cl-ulong)
+    (:device-max-constant-buffer-size                . cl-ulong)
+    (:device-max-constant-args                       . cl-uint)
+    (:device-local-mem-type                          . cl-device-local-mem-type)
+    (:device-local-mem-size                          . cl-ulong)
+    (:device-error-correction-support                . cl-bool)
+    (:device-profiling-timer-resolution              . :size)
+    (:device-endian-little                           . cl-bool)
+    (:device-available                               . cl-bool)
+    (:device-compiler-available                      . cl-bool)
+    (:device-execution-capabilities                  . cl-device-exec-capabilities)
+    (:device-queue-properties                        . cl-command-queue-properties)
+    (:device-queue-on-host-properties                . cl-command-queue-properties)
+    (:device-name                                    . :string)
+    (:device-vendor                                  . :string)
+    (:driver-version                                 . :string)
+    (:device-profile                                 . :string)
+    (:device-version                                 . :string)
+    (:device-extensions                              . :string)
+    (:device-platform                                . cl-platform-id)
+    (:device-double-fp-config                        . cl-device-fp-config)
+    (:device-preferred-vector-width-half             . cl-uint)
+    (:device-host-unified-memory                     . cl-bool)
+    (:device-native-vector-width-char                . cl-uint)
+    (:device-native-vector-width-short               . cl-uint)
+    (:device-native-vector-width-int                 . cl-uint)
+    (:device-native-vector-width-long                . cl-uint)
+    (:device-native-vector-width-float               . cl-uint)
+    (:device-native-vector-width-double              . cl-uint)
+    (:device-native-vector-width-half                . cl-uint)
+    (:device-opencl-c-version                        . :string)
+    (:device-linker-available                        . cl-bool)
+    (:device-built-in-kernels                        . :string)
+    (:device-image-max-buffer-size                   . :size)
+    (:device-image-max-array-size                    . :size)
+    (:device-parent-device                           . cl-device-id)
+    (:device-partition-max-sub-devices               . cl-uint)
+    (:device-partition-properties                    . (:pointer cl-device-partition-property))
+    (:device-partition-affinity-domain               . cl-device-affinity-domain)
+    (:device-partition-type                          . (:pointer cl-device-partition-property))
+    (:device-reference-count                         . cl-uint)
+    (:device-preferred-interop-user-sync             . cl-bool)
+    (:device-printf-buffer-size                      . :size)
+    (:device-image-pitch-alignment                   . cl-uint)
+    (:device-image-base-address-alignment            . cl-uint)
+    (:device-max-read-write-image-args               . cl-uint)
+    (:device-max-global-variable-size                . :size)
+    (:device-queue-on-device-properties              . cl-command-queue-properties)
+    (:device-queue-on-device-preferred-size          . cl-uint)
+    (:device-queue-on-device-max-size                . cl-uint)
+    (:device-max-on-device-queues                    . cl-uint)
+    (:device-max-on-device-events                    . cl-uint)
+    (:device-svm-capabilities                        . cl-device-svm-capabilities)
+    (:device-global-variable-preferred-total-size    . :size)
+    (:device-max-pipe-args                           . cl-uint)
+    (:device-pipe-max-active-reservations            . cl-uint)
+    (:device-pipe-max-packet-size                    . cl-uint)
+    (:device-preferred-platform-atomic-alignment     . cl-uint)
+    (:device-preferred-global-atomic-alignment       . cl-uint)
+    (:device-preferred-local-atomic-alignment        . cl-uint)
+    (:device-il-version                              . :string)
+    (:device-max-num-sub-groups                      . cl-uint)
+    (:device-sub-group-independent-forward-progress  . cl-bool)
+    (:device-numeric-version                         . cl-version)
+    (:device-extensions-with-version                 . (:pointer cl-name-version))
+    (:device-ils-with-version                        . (:pointer cl-name-version))
+    (:device-built-in-kernels-with-version           . (:pointer cl-name-version))
+    (:device-atomic-memory-capabilities              . cl-device-atomic-capabilities)
+    (:device-atomic-fence-capabilities               . cl-device-atomic-capabilities)
+    (:device-non-uniform-work-group-support          . cl-bool)
+    (:device-opencl-c-all-versions                   . (:pointer cl-name-version))
+    (:device-preferred-work-group-size-multiple      . :size)
+    (:device-work-group-collective-functions-support . cl-bool)
+    (:device-generic-address-space-support           . cl-bool)
+    (:device-opencl-c-features                       . (:pointer cl-name-version))
+    (:device-device-enqueue-capabilities             . cl-device-device-enqueue-capabilities)
+    (:device-pipe-support                            . cl-bool)
+    (:device-latest-conformance-version-passed       . :string)))
+
+(wrap-get-info-function get-device-info %get-device-info +device-info-type-alist+)
+
+;; (defun get-device-info (device param-name)
+;;   (let ((type (assoc-value +device-info-type-alist+ param-name))
+;;         (return-size nil)
+;;         (error-code nil)
+;;         (return-value nil))
+;;     (cffi:with-foreign-object (c-return-size :size)
+;;       (setf error-code (%get-device-info device param-name 0 (cffi:null-pointer) c-return-size))
+;;       (unless (eq error-code :success)
+;;         (error 'opencl-error :code error-code))
+;;       (setf return-size (cffi:mem-ref c-return-size :size)))
+;;     (cond ((vector-type-p type)
+;;            (let ((count (/ return-size (cffi:foreign-type-size (second type)))))
+;;              (cffi:with-foreign-object (c-value type count)
+;;                (setf error-code (%get-device-info device param-name return-size c-value (cffi:null-pointer)))
+;;                (setf return-value (loop :for i :below count :collect (cffi:mem-aref c-value type i))) )))
+;;           ((string-type-p type)
+;;            (setf return-value
+;;                  (cffi:with-foreign-pointer-as-string (c-string return-size)
+;;                    (setf error-code (%get-device-info device param-name return-size c-string (cffi:null-pointer))))))
+;;           (t
+;;            (cffi:with-foreign-object (c-value type)
+;;              (setf error-code (%get-device-info device param-name (cffi:foreign-type-size type)
+;;                                                 c-value (cffi:null-pointer)))
+;;              (setf return-value (cffi:mem-ref c-value type)))))
+;;     (unless (eq error-code :success)
+;;       (error 'opencl-error :code error-code))
+;;     return-value))
+
+;; (defun create-sub-devices (in-device properties)
+;;   (check-error (%create-sub-devices in-device )))
+
+(defun retain-device (device)
+  (check-error (%retain-device device)))
+
+(defun release-device (device)
+  (check-error (%release-device device)))
+
+(defun set-default-device-command-queue (context device command-queue)
+  (check-error (%set-default-device-command-queue context device command-queue)))
+
+(defun get-device-and-host-timer (device)
+  (cffi:with-foreign-objects ((device-timestamp 'cl-ulong)
+                              (host-timestamp 'cl-ulong))
+    (check-error (%get-device-and-host-timer device device-timestamp host-timestamp))
+    (values (cffi:mem-ref device-timestamp 'cl-ulong)
+            (cffi:mem-ref host-timestamp 'cl-ulong))))
+
+(defun get-host-timer (device)
+  (cffi:with-foreign-object (host-timestamp 'cl-ulong)
+    (check-error (%get-host-timer device host-timestamp))
+    (cffi:mem-ref host-timestamp 'cl-ulong)))
diff --git a/src/enqueue.lisp b/src/enqueue.lisp
new file mode 100644
index 0000000..d26f1c3
--- /dev/null
+++ b/src/enqueue.lisp
@@ -0,0 +1,77 @@
+(in-package #:ocl)
+
+;; once-only really needed?
+;; gensym really needed?
+(defmacro wrap-enqueue (form event-wait-list)
+  ""
+  (let ((num-events-in-wait-list (gensym "NUM-EVENTS-IN-WAIT-LIST"))
+        (c-event-wait-list (gensym "C-EVENT-WAIT-LIST"))
+        (c-event (gensym "C-EVENT"))
+        (i (gensym "I")))
+    (alexandria:once-only (event-wait-list)
+      `(let ((,num-events-in-wait-list (length ,event-wait-list)))
+         (cffi:with-foreign-object (,c-event 'cl-event)
+           (if (zerop ,num-events-in-wait-list)
+               (check-error (,@form 0 (cffi:null-pointer) ,c-event))
+               (cffi:with-foreign-object (,c-event-wait-list 'cl-event ,num-events-in-wait-list)
+                 (dotimes (,i ,num-events-in-wait-list)
+                   (setf (cffi:mem-aref ,c-event-wait-list 'cl-event ,i) (elt ,event-wait-list ,i)))
+                 (check-error (,@form ,num-events-in-wait-list ,c-event-wait-list ,c-event))
+                 (cffi:mem-ref ,c-event 'cl-event))))))))
+
+(defun enqueue-read-buffer (command-queue buffer blocking-read offset size ptr &optional event-wait-list)
+  (wrap-enqueue (%enqueue-read-buffer command-queue buffer (if blocking-read :true :false) offset size ptr)
+                event-wait-list))
+
+;; TODO: Check dimensions?
+(defun enqueue-nd-range-kernel (queue kernel global-work-offset global-work-size
+                                local-work-size &optional event-wait-list)
+  (setf global-work-offset (alexandria:ensure-list global-work-offset)
+        global-work-size (alexandria:ensure-list global-work-size)
+        local-work-size (alexandria:ensure-list local-work-size))
+  ;; (assert (length global-work-size) ...)
+  (let ((work-dim (length global-work-size)))
+    (with-foreign-sequences ((c-global-work-offset global-work-offset :size)
+                             (c-global-work-size global-work-size :size)
+                             (c-local-work-size local-work-size :size))
+      (wrap-enqueue (%enqueue-nd-range-kernel queue kernel work-dim
+                                              c-global-work-offset c-global-work-size
+                                              c-local-work-size)
+                    event-wait-list))))
+
+(defun enqueue-svm-free (command-queue svm-pointers &optional event-wait-list
+                                                      (pfn-free-func (cffi:null-pointer))
+                                                      (user-data (cffi:null-pointer)))
+  (with-foreign-sequence (c-svm-pointers svm-pointers '(:pointer :void) num-svm-pointers)
+    (wrap-enqueue
+     (%enqueue-svm-free command-queue num-svm-pointers c-svm-pointers
+                        pfn-free-func user-data)
+     event-wait-list)))
+
+(defun enqueue-svm-memcpy (command-queue blocking-copy-p dst-ptr src-ptr size
+                           &optional event-wait-list)
+  (wrap-enqueue
+   (%enqueue-svm-memcpy command-queue (if blocking-copy-p :true :false) dst-ptr src-ptr size)
+   event-wait-list))
+
+(defun enqueue-svm-memfill (command-queue svm-ptr pattern pattern-size size
+                            &optional event-wait-list)
+  (wrap-enqueue
+   (%enqueue-svm-memfill command-queue svm-ptr pattern pattern-size size)
+   event-wait-list))
+
+(defun enqueue-svm-map (command-queue blocking-map-p flags svm-ptr size
+                        &optional event-wait-list)
+  (wrap-enqueue
+   (%enqueue-svm-map command-queue (if blocking-map-p :true :false) flags svm-ptr size)
+   event-wait-list))
+
+(defun enqueue-svm-unmap (command-queue svm-ptr &optional event-wait-list)
+  (wrap-enqueue (%enqueue-svm-unmap command-queue svm-ptr) event-wait-list))
+
+(defun enqueue-svm-migrate-mem (command-queue svm-pointers sizes flags &optional event-wait-list)
+  (assert (or (emptyp sizes) (length= svm-pointers sizes)))
+  (with-foreign-sequences ((c-svm-pointers svm-pointers '(:pointer :void) num-svm-pointers)
+                           (c-sizes sizes :size))
+    (wrap-enqueue (%enqueue-svm-migrate-mem command-queue num-svm-pointers c-svm-pointers c-sizes flags)
+                  event-wait-list)))
diff --git a/src/event.lisp b/src/event.lisp
new file mode 100644
index 0000000..fb6e98a
--- /dev/null
+++ b/src/event.lisp
@@ -0,0 +1,26 @@
+(in-package #:ocl)
+
+(defun wait-for-events (event-list)
+  (with-foreign-sequence (c-event-list event-list 'cl-event num-events)
+    (check-error (%wait-for-events num-events c-event-list))))
+
+(defun create-user-event (context)
+  (check-error-arg (%create-user-event context)))
+
+(defparameter +event-info-type-alist+
+  '((:event-command-queue            . cl-command-queue)
+    (:event-context                  . cl-context)
+    (:event-command-type             . cl-command-type)
+    (:event-command-execution-status . cl-int)
+    (:event-reference-count          . cl-uint)))
+
+(wrap-get-info-function get-event-info %get-event-info +event-info-type-alist+)
+
+(defun retain-event (event)
+  (check-error (%retain-event event)))
+
+(defun release-event (event)
+  (check-error (%release-event event)))
+
+(defun set-user-event-status (event execution-status)
+  (check-error (%set-user-event-status event execution-status)))
diff --git a/src/extensions.lisp b/src/extensions.lisp
new file mode 100644
index 0000000..e69de29
--- /dev/null
+++ b/src/extensions.lisp
diff --git a/src/flush.lisp b/src/flush.lisp
new file mode 100644
index 0000000..4ab282b
--- /dev/null
+++ b/src/flush.lisp
@@ -0,0 +1,7 @@
+(in-package #:ocl)
+
+(defun flush (command-queue)
+  (check-error (%flush command-queue)))
+
+(defun finish (command-queue)
+  (check-error (%finish command-queue)))
diff --git a/src/kernel.lisp b/src/kernel.lisp
new file mode 100644
index 0000000..65bc066
--- /dev/null
+++ b/src/kernel.lisp
@@ -0,0 +1,61 @@
+(in-package #:ocl)
+
+(defun create-kernel (program kernel-name)
+  (check-error-arg (%create-kernel program kernel-name)))
+
+(get-cl-objects create-kernels-in-program (program)
+    %create-kernels-in-program 'cl-kernel)
+
+(defun clone-kernel (source-kernel)
+  (check-error-arg (%clone-kernel source-kernel)))
+
+(defun retain-kernel (kernel)
+  (check-error (%retain-kernel kernel)))
+
+(defun release-kernel (kernel)
+  (check-error (%release-kernel kernel)))
+
+(defmacro with-kernel ((kernel program name) &body body)
+  `(let ((,kernel (create-kernel ,program ,name)))
+     (unwind-protect
+          (progn ,@body)
+       (release-kernel ,kernel))))
+
+(defun set-kernel-arg (kernel arg-index arg-type arg-value)
+  (cffi:with-foreign-pointer (value (cffi:foreign-type-size arg-type) size)
+    (setf (cffi:mem-ref value arg-type) arg-value)
+    (check-error (%set-kernel-arg kernel arg-index size value))))
+
+(defparameter +kernel-info-type-alist+
+  '((:kernel-function-name   . :string)
+    (:kernel-num-args        . cl-uint)
+    (:kernel-reference-count . cl-uint)
+    (:kernel-context         . cl-context)
+    (:kernel-program         . cl-program)
+    (:kernel-attributes      . :string)))
+
+(wrap-get-info-function get-kernel-info %get-kernel-info +kernel-info-type-alist+)
+
+(defparameter +kernel-arg-info-type-alist+
+  '((:kernel-arg-address-qualifier . cl-kernel-arg-address-qualifier)
+    (:kernel-arg-access-qualifier  . cl-kernel-arg-access-qualifier)
+    (:kernel-arg-type-name         . :string)
+    (:kernel-arg-type-qualifier    . cl-kernel-arg-type-qualifier)
+    (:kernel-arg-name              . :string)))
+
+;; %get-kernel-arg-info
+
+(defparameter +kernel-work-group-info-type-alist+
+  '((:kernel-global-work-size                   . (:pointer :size))
+    (:kernel-work-group-size                    . :size)
+    (:kernel-compile-work-group-size            . (:pointer :size))
+    (:kernel-local-mem-size                     . cl-ulong)
+    (:kernel-preferred-work-group-size-multiple . :size)
+    (:kernel-private-mem-size                   . cl-ulong)))
+
+;; %get-kernel-work-group-info
+
+;; (defparameter +kernel-sub-group-info-type-alist+
+;;   '(()))
+
+;; %get-kernel-sub-group-info
diff --git a/src/memory.lisp b/src/memory.lisp
new file mode 100644
index 0000000..f6ab419
--- /dev/null
+++ b/src/memory.lisp
@@ -0,0 +1,89 @@
+(in-package #:ocl)
+
+(defun create-buffer (context flags size &optional (host-ptr (cffi:null-pointer)))
+  (check-error-arg (%create-buffer context flags size host-ptr)))
+
+;; TODO: Support multi-dimensional arrays? row-major?
+(defun create-buffer-from-array (context flags array)
+  (let* ((length (length array))
+         (c-type (array-foreign-type array))
+         (size (* length (cffi:foreign-type-size c-type))))
+    (cffi:with-foreign-array (c-array array (list :array c-type length))
+      (check-error-arg (%create-buffer context flags size c-array)))))
+
+(defun create-pipe (context flags packet-size max-packets &key properties)
+  (declare (ignorable properties))
+  (check-error-arg
+   (%create-pipe context flags packet-size max-packets (cffi:null-pointer))))
+
+(defun retain-mem-object (memobj)
+  (check-error (%retain-mem-object memobj)))
+
+(defun release-mem-object (memobj)
+  (check-error (%release-mem-object memobj)))
+
+(get-cl-objects get-supported-image-formats (context flags image-type)
+                %get-supported-image-formats 'cl-image-format)
+
+(defparameter +mem-object-info-type-alist+
+  '((:mem-type                 . cl-mem-object-type)
+    (:mem-flags                . cl-mem-flags)
+    (:mem-size                 . :size)
+    (:mem-host-ptr             . (:pointer :void))
+    (:mem-map-count            . cl-uint)
+    (:mem-reference-count      . cl-uint)
+    (:mem-context              . cl-context)
+    (:mem-associated-memobject . cl-mem)
+    (:mem-offset               . :size)
+    (:mem-uses-svm-pointer     . cl-bool)
+    (:mem-properties           . (:pointer cl-mem-properties))))
+
+(wrap-get-info-function get-mem-object-info %get-mem-object-info
+                        +mem-object-info-type-alist+)
+
+(defparameter +image-info-type-alist+
+  '((:image-format         . cl-image-format)
+    (:image-element-size   . :size)
+    (:image-row-pitch      . :size)
+    (:image-slice-pitch    . :size)
+    (:image-width          . :size)
+    (:image-height         . :size)
+    (:image-depth          . :size)
+    (:image-array-size     . :size)
+    (:image-buffer         . cl-mem)
+    (:image-num-mip-levels . cl-uint)
+    (:image-num-samples    . cl-uint)))
+
+(wrap-get-info-function get-image-info %get-image-info +image-info-type-alist+)
+
+(defparameter +pipe-info-type-alist+
+  '((:pipe-packet-size . cl-uint)
+    (:pipe-max-packets . cl-uint)
+    (:pipe-properties  . (:pointer cl-pipe-properties))))
+
+(wrap-get-info-function get-pipe-info %get-pipe-info +pipe-info-type-alist+)
+
+(defmacro with-mem-object ())
+
+(defmacro with-buffer ((buffer context flags size &optional host-ptr) &body body)
+  `(let ((,buffer (create-buffer ,context ,flags ,size ,(if host-ptr host-ptr '(cffi:null-pointer)))))
+     (unwind-protect
+          (progn ,@body)
+       (release-mem-object ,buffer))))
+
+(defmacro with-buffer-from-array ((buffer context flags array) &body body)
+  `(let ((,buffer (create-buffer-from-array ,context ,flags ,array)))
+     (unwind-protect
+          (progn ,@body)
+       (release-mem-object ,buffer))))
+
+(defmacro with-buffers-from-arrays ())
+
+(defun copy-buffer-to-array (queue buffer array)
+  (let* ((length (length array))
+         (c-type (array-foreign-type array))
+         (size (* length (cffi:foreign-type-size c-type))))
+    (cffi:with-foreign-object (c-array c-type length)
+      (enqueue-read-buffer queue buffer t 0 size c-array)
+      (dotimes (i length)
+        (setf (aref array i) (cffi:mem-aref c-array c-type i))))))
diff --git a/src/opencl.lisp b/src/opencl.lisp
new file mode 100644
index 0000000..ca95928
--- /dev/null
+++ b/src/opencl.lisp
@@ -0,0 +1,109 @@
+(in-package #:ocl)
+
+(defmacro define-get-info ())
+
+(define-condition opencl-error ()
+  ((code :initarg :code
+          :reader opencl-error-code))
+  (:report (lambda (condition stream)
+             (format stream "OPENCL-ERROR: ~A~%" (opencl-error-code condition)))))
+
+(defmacro check-error (error-code)
+  (alexandria:once-only (error-code)
+    `(unless (eq ,error-code :success)
+       (error 'opencl-error :code ,error-code))))
+
+;; TODO: Finish me
+(defun array-foreign-type (array)
+  "Returns the most appropiate foreign type to store ARRAY"
+  (case (array-element-type array)
+    (single-float :float)
+    (double-float :double)
+    (t nil)))
+
+(defun array-foreign-size (array)
+  "Returns the size in bytes required to store a foreign version of ARRAY"
+  (reduce #'* (array-dimensions array)
+          :initial-value (cffi:foreign-type-size (array-foreign-type array))))
+
+(defmacro check-error-arg (form)
+  (let ((value (gensym "VALUE"))
+        (error-code (gensym "ERROR-CODE"))
+        (c-error-code (gensym "C-ERROR-CODE")))
+    `(cffi:with-foreign-object (,c-error-code 'cl-error-code)
+       (let* ((,value (,@form ,c-error-code))
+              (,error-code (cffi:mem-ref ,c-error-code 'cl-error-code)))
+         (if (eq ,error-code :success)
+             ,value
+             (error 'opencl-error :code ,error-code))))))
+
+(defmacro with-foreign-arrays (bindings &body body)
+  (if (null bindings)
+      `(progn ,@body)
+      `(cffi:with-foreign-array ,(first bindings)
+         (with-foreign-arrays ,(rest bindings)
+           ,@body))))
+
+(defmacro with-foreign-sequence ((var lisp-sequence type &optional length) &body body)
+  "Like CFFI:WITH-FOREIGN-ARRAY but works also for lists"
+  (unless length (setf length (gensym "LENGTH")))
+  (alexandria:once-only (lisp-sequence type)
+    `(let ((,length (length ,lisp-sequence)))
+       (cffi:with-foreign-object (,var ,type ,length)
+         (dotimes (i ,length)
+           (setf (cffi:mem-aref ,var ,type i) (elt ,lisp-sequence i)))
+         ,@body))))
+
+(defmacro with-foreign-sequences (bindings &body body)
+  (if bindings
+      `(with-foreign-sequence ,(first bindings)
+         (with-foreign-sequences ,(rest bindings)
+           ,@body))
+      `(progn ,@body)))
+
+(defun vector-type-p (type)
+  (and (consp type) (eq (car type) :pointer)))
+
+(defun string-type-p (type)
+  (eq type :string))
+
+(defmacro wrap-get-info-function (name low-level-name type-alist)
+  ""
+  ;; FIXME? This is a top level form, no call to GENSYM is needed, right?
+  `(defun ,name (object param-name)
+     (let ((type (assoc-value ,type-alist param-name))
+           (return-size nil)
+           (error-code nil)
+           (return-value nil))
+       (cffi:with-foreign-object (c-return-size :size)
+         (setf error-code (,low-level-name object param-name 0 (cffi:null-pointer) c-return-size))
+         (check-error error-code)
+         (setf return-size (cffi:mem-ref c-return-size :size)))
+       (cond ((vector-type-p type)
+              (let ((count (/ return-size (cffi:foreign-type-size (second type)))))
+                (cffi:with-foreign-object (c-value type count)
+                  (setf error-code (,low-level-name object param-name return-size c-value (cffi:null-pointer)))
+                  (setf return-value (loop :for i :below count :collect (cffi:mem-aref c-value type i))))))
+             ((string-type-p type)
+              (setf return-value
+                    (cffi:with-foreign-pointer-as-string (c-string return-size)
+                      (setf error-code (,low-level-name object param-name return-size c-string (cffi:null-pointer))))))
+             (t
+              (cffi:with-foreign-object (c-value type)
+                (setf error-code (,low-level-name object param-name (cffi:foreign-type-size type)
+                                                  c-value (cffi:null-pointer)))
+                (setf return-value (cffi:mem-ref c-value type)))))
+       (check-error error-code)
+       return-value)))
+
+(defmacro get-cl-objects (name (&rest args) low-level-name type)
+  (assert (every #'symbolp args) nil "ARGS must be a list of only symbols")
+  `(defun ,name (,@args)
+     (let (n)
+       (cffi:with-foreign-object (cn 'cl-uint)
+         (check-error (,low-level-name ,@args 0 (cffi:null-pointer) cn))
+         (setf n (cffi:mem-ref cn 'cl-uint)))
+       (cffi:with-foreign-object (c-objects ,type n)
+         (check-error (,low-level-name ,@args n c-objects (cffi:null-pointer)))
+         (loop :for i :below n
+               :collect (cffi:mem-aref c-objects ,type i))))))
diff --git a/src/package.lisp b/src/package.lisp
new file mode 100644
index 0000000..ce8dc38
--- /dev/null
+++ b/src/package.lisp
@@ -0,0 +1,247 @@
+(defpackage #:ocl-ffi
+  (:use #:cl)
+  (:export
+   ;; Platform APIs
+   %get-platform-ids
+   %get-platform-info
+
+   ;; Device APIs
+   %get-device-ids
+   %get-device-info
+   %create-sub-devices
+   %retain-device
+   %release-device
+   %set-default-device-command-queue
+   %get-device-and-host-timer
+   %get-host-timer
+
+   ;; Context APIs
+   %create-context
+   %create-context-from-type
+   %retain-context
+   %release-context
+   %get-context-info
+   set-context-destructor-callback
+
+   ;; Command Queue APIs
+   %create-command-queue-with-properties
+   %retain-command-queue
+   %release-command-queue
+   %get-command-queue-info
+
+   ;; Memory Object APIs
+   %create-buffer
+   create-sub-buffer
+   create-image
+   %create-pipe
+   create-buffer-with-properties
+   create-image-with-properties
+   %retain-mem-object
+   %release-mem-object
+   %get-supported-image-formats
+   %get-mem-object-info
+   %get-image-info
+   %get-pipe-info
+   set-mem-object-destructor-callback
+
+   ;; SVM Allocation APIs
+   svm-alloc
+   svm-free
+
+   ;; Sampler APIs
+   %create-sampler-with-properties
+   %retain-sampler
+   %release-sampler
+   %get-sampler-info
+
+   ;; Program Object APIs
+   %create-program-with-source
+   create-program-with-binary
+   create-program-with-built-in-kernels
+   create-program-with-il
+   %retain-program
+   %release-program
+   %build-program
+   %compile-program
+   %link-program
+   set-program-release-callback
+   set-program-specialization-constant
+   %unload-platform-compiler
+   %get-program-info
+   %get-program-build-info
+
+   ;; Kernel Object APIs
+   %create-kernel
+   %create-kernels-in-program
+   %clone-kernel
+   %retain-kernel
+   %release-kernel
+   %set-kernel-arg
+   set-kernel-arg-svm-pointer
+   set-kernel-exec-info
+   %get-kernel-info
+   %get-kernel-arg-info
+   %get-kernel-work-group-info
+   %get-kernel-sub-group-info
+
+   ;; Event Object APIs
+   %wait-for-events
+   %get-event-info
+   %create-user-event
+   %retain-event
+   %release-event
+   %set-user-event-status
+   set-event-callback
+
+   ;; Profiling APIs
+   %get-event-profiling-info
+
+   ;; Flush and Finish APIs
+   %flush
+   %finish
+
+   ;; Enqueued Commands APIs
+   %enqueue-read-buffer
+   enqueue-read-buffer-rect
+   enqueue-write-buffer
+   enqueue-write-buffer-rect
+   enqueue-fill-buffer
+   enqueue-copy-buffer
+   enqueue-copy-buffer-rect
+   enqueue-read-image
+   enqueue-write-image
+   enqueue-fill-image
+   enqueue-copy-image
+   enqueue-copy-image-to-buffer
+   enqueue-copy-buffer-to-image
+   enqueue-map-buffer
+   enqueue-map-image
+   enqueue-unmap-mem-object
+   enqueue-migrate-mem-objects
+   %enqueue-nd-range-kernel
+   enqueue-native-kernel
+   enqueue-marker-with-wait-list
+   enqueue-barrier-with-wait-list
+   %enqueue-svm-free
+   %enqueue-svm-memcpy
+   %enqueue-svm-memfill
+   %enqueue-svm-map
+   %enqueue-svm-unmap
+   %enqueue-svm-migrate-mem
+
+   ;; Extension function access
+   get-extension-function-address-for-platform
+
+   ;; Deprecated OpenCL 1.0 APIs
+   set-command-queue-property
+
+   ;; Deprecated OpenCL 1.1 APIs
+   create-image-2d
+   create-image-3d
+   enqueue-marker
+   %enqueue-wait-for-events
+   enqueue-barrier
+   unload-compiler
+   get-extension-function-address
+
+   ;; Deprecated OpenCL 2.0 APIs
+   %create-command-queue
+   create-sampler
+   enqueue-task
+
+   ;; Types
+   cl-char
+   cl-uchar
+   cl-short
+   cl-ushort
+   cl-int
+   cl-uint
+   cl-long
+   cl-ulong
+
+   cl-half
+   cl-float
+   cl-double
+
+   cl-platform-id
+   cl-device-id
+   cl-context
+   cl-command-queue
+   cl-mem
+   cl-program
+   cl-kernel
+   cl-event
+   cl-sampler
+
+   cl-error-code
+   cl-bool
+   cl-bitfield
+   cl-properties
+
+   cl-platform-info
+   cl-device-info
+
+   cl-device-mem-cache-type
+   cl-device-local-mem-type
+   cl-context-info
+   cl-command-queue-info
+   cl-channel-order
+   cl-channel-type
+   cl-mem-object-type
+   cl-mem-info
+   cl-image-info
+   cl-pipe-info
+   cl-addressing-mode
+   cl-filter-mode
+   cl-sampler-info
+   cl-program-info
+   cl-program-build-info
+   cl-build-status
+   cl-kernel-info
+   cl-kernel-arg-info
+   cl-kernel-arg-address-qualifier
+   cl-kernel-arg-access-qualifier
+   cl-kernel-work-group-info
+   cl-kernel-sub-group-info
+   cl-kernel-exec-info
+   cl-event-info
+   cl-command-type
+   cl-buffer-create-type
+   cl-profiling-info
+   cl-khronos-vendor-id
+   cl-device-type
+   cl-device-fp-config
+   cl-device-exec-capabilities
+   cl-device-svm-capabilities
+   cl-command-queue-properties
+   cl-device-affinity-domain
+   cl-mem-flags
+   cl-svm-mem-flags
+   cl-mem-migration-flags
+   cl-program-binary-type
+   cl-map-flags
+   cl-kernel-arg-type-qualifier
+   cl-device-atomic-capabilities
+   cl-device-device-enqueue-capabilities
+   cl-mem-properties
+   cl-queue-properties
+   cl-device-partition-property
+   cl-context-properties
+   cl-pipe-properties
+   cl-sampler-properties
+   cl-version
+   cl-image-format
+   cl-buffer-region
+   cl-name-version
+   cl-image-desc))
+
+(defpackage #:ocl
+   (:use #:cl #:alexandria #:ocl-ffi))
+
+(in-package #:ocl)
+
+(cffi:define-foreign-library libopencl
+  (:unix (:or "libOpenCL.so" "/gnu/store/i70jq190cpc45crbnrw8g8lgb4djyi9r-opencl-icd-loader-2021.06.30/lib/libOpenCL.so"))
+  (t (:default "libOpenCL")))
+
+(cffi:use-foreign-library libopencl)
diff --git a/src/platform.lisp b/src/platform.lisp
new file mode 100644
index 0000000..1b976f4
--- /dev/null
+++ b/src/platform.lisp
@@ -0,0 +1,24 @@
+(in-package #:ocl)
+
+(defun get-platform-ids ()
+  (let ((num-platforms nil))
+    (cffi:with-foreign-object (c-num-platforms 'cl-uint)
+      (check-error (%get-platform-ids 0 (cffi:null-pointer) c-num-platforms))
+      (setf num-platforms (cffi:mem-ref c-num-platforms 'cl-uint)))
+    (cffi:with-foreign-object (c-platforms 'cl-platform-id num-platforms)
+      (check-error (%get-platform-ids num-platforms c-platforms (cffi:null-pointer)))
+      (loop :for i :below num-platforms
+            :collect (cffi:mem-aref c-platforms 'cl-platform-id i)))))
+
+(defparameter +platform-info-type-alist+
+  '((:platform-profile                 . :string)
+    (:platform-version                 . :string)
+    (:platform-numeric-version         . cl-version)
+    (:platform-name                    . :string)
+    (:platform-vendor                  . :string)
+    (:platform-extensions              . :string)
+    (:platform-extensions-with-version . (:pointer cl-name-version))
+    (:platform-host-timer-resolution   . cl-ulong)))
+
+(wrap-get-info-function get-platform-info %get-platform-info
+                        +platform-info-type-alist+)
diff --git a/src/profiling.lisp b/src/profiling.lisp
new file mode 100644
index 0000000..2d186d6
--- /dev/null
+++ b/src/profiling.lisp
@@ -0,0 +1,11 @@
+(in-package #:ocl)
+
+(defparameter +event-profiling-info-type-alist+
+  '((:profiling-command-queued   . cl-ulong)
+    (:profiling-command-submit   . cl-ulong)
+    (:profiling-command-start    . cl-ulong)
+    (:profiling-command-end      . cl-ulong)
+    (:profiling-command-complete . cl-ulong)))
+
+(wrap-get-info-function get-event-profiling-info %get-event-profiling-info
+                        +event-profiling-info-type-alist+)
diff --git a/src/program.lisp b/src/program.lisp
new file mode 100644
index 0000000..4f27a25
--- /dev/null
+++ b/src/program.lisp
@@ -0,0 +1,83 @@
+(in-package #:ocl)
+
+(defun create-program-with-source (context list-of-strings)
+  (setf list-of-strings (alexandria:ensure-list list-of-strings))
+  (let ((num-strings (length list-of-strings)))
+    (cffi:with-foreign-object (c-strings :pointer num-strings)
+      (dotimes (i num-strings)
+        (setf (cffi:mem-aref c-strings :pointer i)
+              (cffi:foreign-string-alloc (elt list-of-strings i))))
+      (unwind-protect
+           (check-error-arg (%create-program-with-source context num-strings c-strings (cffi:null-pointer)))
+        (dotimes (i num-strings)
+          (cffi:foreign-string-free (cffi:mem-aref c-strings :pointer i)))))))
+
+(defun retain-program (program)
+  (check-error (%retain-program program)))
+
+(defun release-program (program)
+  (%release-program program))
+
+(defun build-program (program device-list &key (options (cffi:null-pointer))
+                                            (pfn-notify (cffi:null-pointer))
+                                            (user-data (cffi:null-pointer)))
+  (setf device-list (alexandria:ensure-list device-list))
+  (with-foreign-sequence (c-devices device-list 'cl-device-id num-devices)
+    (check-error (%build-program program num-devices c-devices options
+                                 pfn-notify user-data))))
+
+;; (defun compile-program (program device-list
+;;                         &key (options (cffi:null-pointer))
+;;                           input-headers
+;;                           header-include-names
+;;                           (pfn-notify (cffi:null-pointer))
+;;                           (user-data (cffi:null-pointer)))
+;;   (with-foreign-sequence ((c-device-list device-list 'cl-device-id num-devices)
+;;                           (c-input-headers input-headers 'cl-program num-input-headers))
+;;     (check-error (%compile-program program num-devices c-device-list options
+;;                                    num-input-headers c-input-headers
+;;                                    pfn-notify user-data))))
+
+(defun link-program (context device-list input-programs &key (options (cffi:null-pointer))
+                                                          (pfn-notify (cffi:null-pointer))
+                                                          (user-data (cffi:null-pointer)))
+  (assert (not (emptyp input-programs)))
+  (with-foreign-sequences ((c-device-list device-list 'cl-device-id num-devices)
+                           (c-input-programs input-programs 'cl-program num-input-programs))
+    (check-error-arg (%link-program context num-devices c-device-list options
+                                    num-input-programs c-input-programs
+                                    pfn-notify user-data))))
+
+(defun unload-platform-compiler (platform)
+  (check-error (%unload-platform-compiler platform)))
+
+(defparameter +program-info-type-alist+
+  '((:program-reference-count            . cl-uint)
+    (:program-context                    . cl-context)
+    (:program-num-devices                . cl-uint)
+    (:program-devices                    . (:pointer cl-device-id))
+    (:program-source                     . :string)
+    (:program-il                         . (:pointer :char))
+    (:program-binary-sizes               . (:pointer :size))
+    (:program-binaries                   . (:pointer (:pointer :char)))
+    (:program-num-kernels                . :size)
+    (:program-kernel-names               . (:pointer :char))
+    (:program-scope-global-ctors-present . cl-bool)
+    (:program-scope-global-dtors-present . cl-bool)))
+
+;; %get-program-info
+
+(defparameter +program-build-info-type-alist+
+  '((:program-build-status                     . cl-build-status)
+    (:program-build-options                    . :string)
+    (:program-build-log                        . :string)
+    (:program-binary-type                      . cl-program-binary-type)
+    (:program-build-global-variable-total-size . :size)))
+
+;; %get-program-build-info
+
+(defmacro with-program-from-source ((program context list-of-strings) &body body)
+  `(let ((,program (create-program-with-source ,context ,list-of-strings)))
+     (unwind-protect
+          (progn ,@body)
+       (release-program ,program))))
diff --git a/src/sampler.lisp b/src/sampler.lisp
new file mode 100644
index 0000000..5521ed7
--- /dev/null
+++ b/src/sampler.lisp
@@ -0,0 +1,27 @@
+(in-package #:ocl)
+
+(defun create-sampler-with-properties (context &key (normalized-coords-p t)
+                                                 (addressing-mode :address-clamp)
+                                                 (filter-mode :filter-nearest))
+  (let ((properties `(:sampler-normalized-coords ,normalized-coords-p
+                      :sampler-addressing-mode ,addressing-mode
+                      :sampler-filter-mode ,filter-mode
+                      0)))
+    (with-foreign-sequence (c-properties properties 'cl-sampler-properties)
+      (check-error-arg (%create-sampler-with-properties context sampler-properties)))))
+
+(defun retain-sampler (sampler)
+  (check-error (%retain-sampler sampler)))
+
+(defun release-sampler (sampler)
+  (check-error (%release-sampler sampler)))
+
+(defparameter +sampler-info-type-alist+
+  '((:sampler-reference-count   . cl-uint)
+    (:sampler-context           . cl-context)
+    (:sampler-normalized-coords . cl-bool)
+    (:sampler-addressing-mode   . cl-addressing-mode)
+    (:sampler-filter-mode       . cl-filter-mode)
+    (:sampler-properties        . (:pointer cl-sampler-properties))))
+
+(wrap-get-info-function get-sampler-info %get-sampler-info +sampler-info-type-alist+)
diff --git a/src/types.lisp b/src/types.lisp
new file mode 100644
index 0000000..20a4882
--- /dev/null
+++ b/src/types.lisp
@@ -0,0 +1,630 @@
+(in-package #:ocl-ffi)
+
+(cffi:defctype cl-char :int8)
+(cffi:defctype cl-uchar :uint8)
+(cffi:defctype cl-short :int16)
+(cffi:defctype cl-ushort :uint16)
+(cffi:defctype cl-int :int32)
+(cffi:defctype cl-uint :uint32)
+(cffi:defctype cl-long :int64)
+(cffi:defctype cl-ulong :uint64)
+
+(cffi:defctype cl-half :uint16)
+(cffi:defctype cl-float :float)
+(cffi:defctype cl-double :double)
+
+(cffi:defctype cl-platform-id :pointer)
+(cffi:defctype cl-device-id :pointer)
+(cffi:defctype cl-context :pointer)
+(cffi:defctype cl-command-queue :pointer)
+(cffi:defctype cl-mem :pointer)
+(cffi:defctype cl-program :pointer)
+(cffi:defctype cl-kernel :pointer)
+(cffi:defctype cl-event :pointer)
+(cffi:defctype cl-sampler :pointer)
+
+;;; Error Codes
+(cffi:defcenum (cl-error-code cl-int)
+  (:complete                                  0)
+  (:running                                   1)
+  (:submitted                                 2)
+  (:queued                                    3)
+  (:success                                   0)
+  (:device-not-found                         -1)
+  (:device-not-available                     -2)
+  (:compiler-not-available                   -3)
+  (:mem-object-allocation-failure            -4)
+  (:out-of-resources                         -5)
+  (:out-of-host-memory                       -6)
+  (:profiling-info-not-available             -7)
+  (:mem-copy-overlap                         -8)
+  (:image-format-mismatch                    -9)
+  (:image-format-not-supported               -10)
+  (:build-program-failure                    -11)
+  (:map-failure                              -12)
+  (:misaligned-sub-buffer-offset             -13)
+  (:exec-status-error-for-events-in-wait-list -14)
+  (:compile-program-failure                  -15)
+  (:linker-not-available                     -16)
+  (:link-program-failure                     -17)
+  (:device-partition-failed                  -18)
+  (:kernel-arg-info-not-available            -19)
+  (:invalid-value                            -30)
+  (:invalid-device-type                      -31)
+  (:invalid-platform                         -32)
+  (:invalid-device                           -33)
+  (:invalid-context                          -34)
+  (:invalid-queue-properties                 -35)
+  (:invalid-command-queue                    -36)
+  (:invalid-host-ptr                         -37)
+  (:invalid-mem-object                       -38)
+  (:invalid-image-format-descriptor          -39)
+  (:invalid-image-size                       -40)
+  (:invalid-sampler                          -41)
+  (:invalid-binary                           -42)
+  (:invalid-build-options                    -43)
+  (:invalid-program                          -44)
+  (:invalid-program-executable               -45)
+  (:invalid-kernel-name                      -46)
+  (:invalid-kernel-definition                -47)
+  (:invalid-kernel                           -48)
+  (:invalid-arg-index                        -49)
+  (:invalid-arg-value                        -50)
+  (:invalid-arg-size                         -51)
+  (:invalid-kernel-args                      -52)
+  (:invalid-work-dimension                   -53)
+  (:invalid-work-group-size                  -54)
+  (:invalid-work-item-size                   -55)
+  (:invalid-global-offset                    -56)
+  (:invalid-event-wait-list                  -57)
+  (:invalid-event                            -58)
+  (:invalid-operation                        -59)
+  (:invalid-gl-object                        -60)
+  (:invalid-buffer-size                      -61)
+  (:invalid-mip-level                        -62)
+  (:invalid-global-work-size                 -63)
+  (:invalid-property                         -64)
+  (:invalid-image-descriptor                 -65)
+  (:invalid-compiler-options                 -66)
+  (:invalid-linker-options                   -67)
+  (:invalid-device-partition-count           -68)
+  (:invalid-pipe-size                        -69)
+  (:invalid-device-queue                     -70)
+  (:invalid-spec-id                          -71)
+  (:max-size-restriction-exceeded            -72))
+
+(cffi:defcenum (cl-bool cl-uint)
+  (:false 0)
+  (:true 1)
+  (:blocking 1)
+  (:non-blocking 0))
+
+(cffi:defctype cl-bitfield cl-ulong)
+(cffi:defctype cl-properties cl-ulong)
+
+(cffi:defcenum (cl-platform-info cl-uint)
+  (:platform-profile #x0900)
+  (:platform-version #x0901)
+  (:platform-name #x0902)
+  (:platform-vendor #x0903)
+  (:platform-extensions #x0904)
+  (:platform-host-timer-resolution #x0905)
+  (:platform-numeric-version #x0906)
+  (:platform-extensions-with-version #x0907))
+
+(cffi:defcenum (cl-device-info cl-uint)
+  (:device-type #x1000)
+  (:device-vendor-id #x1001)
+  (:device-max-compute-units #x1002)
+  (:device-max-work-item-dimensions #x1003)
+  (:device-max-work-group-size #x1004)
+  (:device-max-work-item-sizes #x1005)
+  (:device-preferred-vector-width-char #x1006)
+  (:device-preferred-vector-width-short #x1007)
+  (:device-preferred-vector-width-int #x1008)
+  (:device-preferred-vector-width-long #x1009)
+  (:device-preferred-vector-width-float #x100a)
+  (:device-preferred-vector-width-double #x100b)
+  (:device-max-clock-frequency #x100c)
+  (:device-address-bits #x100d)
+  (:device-max-read-image-args #x100e)
+  (:device-max-write-image-args #x100f)
+  (:device-max-mem-alloc-size #x1010)
+  (:device-image2d-max-width #x1011)
+  (:device-image2d-max-height #x1012)
+  (:device-image3d-max-width #x1013)
+  (:device-image3d-max-height #x1014)
+  (:device-image3d-max-depth #x1015)
+  (:device-image-support #x1016)
+  (:device-max-parameter-size #x1017)
+  (:device-max-samplers #x1018)
+  (:device-mem-base-addr-align #x1019)
+  (:device-min-data-type-align-size #x101a)
+  (:device-single-fp-config #x101b)
+  (:device-global-mem-cache-type #x101c)
+  (:device-global-mem-cacheline-size #x101d)
+  (:device-global-mem-cache-size #x101e)
+  (:device-global-mem-size #x101f)
+  (:device-max-constant-buffer-size #x1020)
+  (:device-max-constant-args #x1021)
+  (:device-local-mem-type #x1022)
+  (:device-local-mem-size #x1023)
+  (:device-error-correction-support #x1024)
+  (:device-profiling-timer-resolution #x1025)
+  (:device-endian-little #x1026)
+  (:device-available #x1027)
+  (:device-compiler-available #x1028)
+  (:device-execution-capabilities #x1029)
+  (:device-queue-properties #x102a)
+  (:device-queue-on-host-properties #x102a)
+  (:device-name #x102b)
+  (:device-vendor #x102c)
+  (:driver-version #x102d)
+  (:device-profile #x102e)
+  (:device-version #x102f)
+  (:device-extensions #x1030)
+  (:device-platform #x1031)
+  (:device-double-fp-config #x1032)
+  (:device-preferred-vector-width-half #x1034)
+  (:device-host-unified-memory #x1035)
+  (:device-native-vector-width-char #x1036)
+  (:device-native-vector-width-short #x1037)
+  (:device-native-vector-width-int #x1038)
+  (:device-native-vector-width-long #x1039)
+  (:device-native-vector-width-float #x103a)
+  (:device-native-vector-width-double #x103b)
+  (:device-native-vector-width-half #x103c)
+  (:device-opencl-c-version #x103d)
+  (:device-linker-available #x103e)
+  (:device-built-in-kernels #x103f)
+  (:device-image-max-buffer-size #x1040)
+  (:device-image-max-array-size #x1041)
+  (:device-parent-device #x1042)
+  (:device-partition-max-sub-devices #x1043)
+  (:device-partition-properties #x1044)
+  (:device-partition-affinity-domain #x1045)
+  (:device-partition-type #x1046)
+  (:device-reference-count #x1047)
+  (:device-preferred-interop-user-sync #x1048)
+  (:device-printf-buffer-size #x1049)
+  (:device-image-pitch-alignment #x104a)
+  (:device-image-base-address-alignment #x104b)
+  (:device-max-read-write-image-args #x104c)
+  (:device-max-global-variable-size #x104d)
+  (:device-queue-on-device-properties #x104e)
+  (:device-queue-on-device-preferred-size #x104f)
+  (:device-queue-on-device-max-size #x1050)
+  (:device-max-on-device-queues #x1051)
+  (:device-max-on-device-events #x1052)
+  (:device-svm-capabilities #x1053)
+  (:device-global-variable-preferred-total-size #x1054)
+  (:device-max-pipe-args #x1055)
+  (:device-pipe-max-active-reservations #x1056)
+  (:device-pipe-max-packet-size #x1057)
+  (:device-preferred-platform-atomic-alignment #x1058)
+  (:device-preferred-global-atomic-alignment #x1059)
+  (:device-preferred-local-atomic-alignment #x105a)
+  (:device-il-version #x105b)
+  (:device-max-num-sub-groups #x105c)
+  (:device-sub-group-independent-forward-progress #x105d)
+  (:device-numeric-version #x105e)
+  (:device-extensions-with-version #x1060)
+  (:device-ils-with-version #x1061)
+  (:device-built-in-kernels-with-version #x1062)
+  (:device-atomic-memory-capabilities #x1063)
+  (:device-atomic-fence-capabilities #x1064)
+  (:device-non-uniform-work-group-support #x1065)
+  (:device-opencl-c-all-versions #x1066)
+  (:device-preferred-work-group-size-multiple #x1067)
+  (:device-work-group-collective-functions-support #x1068)
+  (:device-generic-address-space-support #x1069)
+  (:device-opencl-c-features #x106f)
+  (:device-device-enqueue-capabilities #x1070)
+  (:device-pipe-support #x1071)
+  (:device-latest-conformance-version-passed #x1072))
+
+(cffi:defcenum (cl-device-mem-cache-type cl-uint)
+  (:none #x0)
+  (:read-only-cache #x1)
+  (:read-write-cache #x2))
+
+(cffi:defcenum (cl-device-local-mem-type cl-uint)
+  (:local #x1)
+  (:global #x2))
+
+
+(cffi:defcenum (cl-context-info cl-uint)
+  (:context-reference-count #x1080)
+  (:context-devices #x1081)
+  (:context-properties #x1082)
+  (:context-num-devices #x1083))
+
+(cffi:defcenum (cl-command-queue-info cl-uint)
+  (:queue-context #x1090)
+  (:queue-device #x1091)
+  (:queue-reference-count #x1092)
+  (:queue-properties #x1093)
+  (:queue-size #x1094)
+  (:queue-device-default #x1095)
+  (:queue-properties-array #x1098))
+
+(cffi:defcenum (cl-channel-order cl-uint)
+  (:r #x10b0)
+  (:a #x10b1)
+  (:rg #x10b2)
+  (:ra #x10b3)
+  (:rgb #x10b4)
+  (:rgba #x10b5)
+  (:bgra #x10b6)
+  (:argb #x10b7)
+  (:intensity #x10b8)
+  (:luminance #x10b9)
+  (:rx #x10ba)
+  (:rgx #x10bb)
+  (:rgbx #x10bc)
+  (:depth #x10bd)
+  (:depth-stencil #x10be)
+  (:srgb #x10bf)
+  (:srgbx #x10c0)
+  (:srgba #x10c1)
+  (:sbgra #x10c2)
+  (:abgr #x10c3))
+
+(cffi:defcenum (cl-channel-type cl-uint)
+  (:snorm-int8 #x10d0)
+  (:snorm-int16 #x10d1)
+  (:unorm-int8 #x10d2)
+  (:unorm-int16 #x10d3)
+  (:unorm-short-565 #x10d4)
+  (:unorm-short-555 #x10d5)
+  (:unorm-int-101010 #x10d6)
+  (:signed-int8 #x10d7)
+  (:signed-int16 #x10d8)
+  (:signed-int32 #x10d9)
+  (:unsigned-int8 #x10da)
+  (:unsigned-int16 #x10db)
+  (:unsigned-int32 #x10dc)
+  (:half-float #x10dd)
+  (:float #x10de)
+  (:unorm-int24 #x10df)
+  (:unorm-int-101010-2 #x10e0))
+
+(cffi:defcenum (cl-mem-object-type cl-uint)
+  (:mem-object-buffer #x10f0)
+  (:mem-object-image2d #x10f1)
+  (:mem-object-image3d #x10f2)
+  (:mem-object-image2d-array #x10f3)
+  (:mem-object-image1d #x10f4)
+  (:mem-object-image1d-array #x10f5)
+  (:mem-object-image1d-buffer #x10f6)
+  (:mem-object-pipe #x10f7))
+
+(cffi:defcenum (cl-mem-info cl-uint)
+  (:mem-type #x1100)
+  (:mem-flags #x1101)
+  (:mem-size #x1102)
+  (:mem-host-ptr #x1103)
+  (:mem-map-count #x1104)
+  (:mem-reference-count #x1105)
+  (:mem-context #x1106)
+  (:mem-associated-memobject #x1107)
+  (:mem-offset #x1108)
+  (:mem-uses-svm-pointer #x1109)
+  (:mem-properties #x110a))
+
+(cffi:defcenum (cl-image-info cl-uint)
+  (:image-format #x1110)
+  (:image-element-size #x1111)
+  (:image-row-pitch #x1112)
+  (:image-slice-pitch #x1113)
+  (:image-width #x1114)
+  (:image-height #x1115)
+  (:image-depth #x1116)
+  (:image-array-size #x1117)
+  (:image-buffer #x1118)
+  (:image-num-mip-levels #x1119)
+  (:image-num-samples #x111a))
+
+(cffi:defcenum (cl-pipe-info cl-uint)
+  (:pipe-packet-size #x1120)
+  (:pipe-max-packets #x1121)
+  (:pipe-properties #x1122))
+
+(cffi:defcenum (cl-addressing-mode cl-uint)
+  (:address-none #x1130)
+  (:address-clamp-to-edge #x1131)
+  (:address-clamp #x1132)
+  (:address-repeat #x1133)
+  (:address-mirrored-repeat #x1134))
+
+(cffi:defcenum (cl-filter-mode cl-uint)
+  (:filter-nearest #x1140)
+  (:filter-linear #x1141))
+
+(cffi:defcenum (cl-sampler-info cl-uint)
+  (:sampler-reference-count #x1150)
+  (:sampler-context #x1151)
+  (:sampler-normalized-coords #x1152)
+  (:sampler-addressing-mode #x1153)
+  (:sampler-filter-mode #x1154)
+  (:sampler-mip-filter-mode #x1155)
+  (:sampler-lod-min #x1156)
+  (:sampler-lod-max #x1157)
+  (:sampler-properties #x1158))
+
+(cffi:defcenum (cl-program-info cl-uint)
+  (:program-reference-count #x1160)
+  (:program-context #x1161)
+  (:program-num-devices #x1162)
+  (:program-devices #x1163)
+  (:program-source #x1164)
+  (:program-binary-sizes #x1165)
+  (:program-binaries #x1166)
+  (:program-num-kernels #x1167)
+  (:program-kernel-names #x1168)
+  (:program-il #x1169)
+  (:program-scope-global-ctors-present #x116a)
+  (:program-scope-global-dtors-present #x116b))
+
+(cffi:defcenum (cl-program-build-info cl-uint)
+  (:program-build-status #x1181)
+  (:program-build-options #x1182)
+  (:program-build-log #x1183)
+  (:program-binary-type #x1184)
+  (:program-build-global-variable-total-size #x1185))
+
+(cffi:defcenum (cl-build-status cl-int)
+  (:build-success 0)
+  (:build-none -1)
+  (:build-error -2)
+  (:build-in-progress -3))
+
+(cffi:defcenum (cl-kernel-info cl-uint)
+  (:kernel-function-name #x1190)
+  (:kernel-num-args #x1191)
+  (:kernel-reference-count #x1192)
+  (:kernel-context #x1193)
+  (:kernel-program #x1194)
+  (:kernel-attributes #x1195))
+
+(cffi:defcenum (cl-kernel-arg-info cl-uint)
+  (:kernel-arg-address-qualifier #x1196)
+  (:kernel-arg-access-qualifier #x1197)
+  (:kernel-arg-type-name #x1198)
+  (:kernel-arg-type-qualifier #x1199)
+  (:kernel-arg-name #x119a))
+
+(cffi:defcenum (cl-kernel-arg-address-qualifier cl-uint)
+  (:kernel-arg-address-global #x119b)
+  (:kernel-arg-address-local #x119c)
+  (:kernel-arg-address-constant #x119d)
+  (:kernel-arg-address-private #x119e))
+
+(cffi:defcenum (cl-kernel-arg-access-qualifier cl-uint)
+  (:kernel-arg-access-read-only #x11a0)
+  (:kernel-arg-access-write-only #x11a1)
+  (:kernel-arg-access-read-write #x11a2)
+  (:kernel-arg-access-none #x11a3))
+
+(cffi:defcenum (cl-kernel-work-group-info cl-uint)
+  (:kernel-work-group-size #x11b0)
+  (:kernel-compile-work-group-size #x11b1)
+  (:kernel-local-mem-size #x11b2)
+  (:kernel-preferred-work-group-size-multiple #x11b3)
+  (:kernel-private-mem-size #x11b4)
+  (:kernel-global-work-size #x11b5))
+
+(cffi:defcenum (cl-kernel-sub-group-info cl-uint)
+  (:kernel-max-sub-group-size-for-ndrange #x2033)
+  (:kernel-sub-group-count-for-ndrange #x2034)
+  (:kernel-local-size-for-sub-group-count #x11b8)
+  (:kernel-max-num-sub-groups #x11b9)
+  (:kernel-compile-num-sub-groups #x11ba))
+
+(cffi:defcenum (cl-kernel-exec-info cl-uint)
+  (:kernel-exec-info-svm-ptrs #x11b6)
+  (:kernel-exec-info-svm-fine-grain-system #x11b7))
+
+
+(cffi:defcenum (cl-event-info cl-uint)
+  (:event-command-queue #x11d0)
+  (:event-command-type #x11d1)
+  (:event-reference-count #x11d2)
+  (:event-command-execution-status #x11d3)
+  (:event-context #x11d4))
+
+(cffi:defcenum (cl-command-type cl-uint)
+  (:command-ndrange-kernel #x11f0)
+  (:command-task #x11f1)
+  (:command-native-kernel #x11f2)
+  (:command-read-buffer #x11f3)
+  (:command-write-buffer #x11f4)
+  (:command-copy-buffer #x11f5)
+  (:command-read-image #x11f6)
+  (:command-write-image #x11f7)
+  (:command-copy-image #x11f8)
+  (:command-copy-image-to-buffer #x11f9)
+  (:command-copy-buffer-to-image #x11fa)
+  (:command-map-buffer #x11fb)
+  (:command-map-image #x11fc)
+  (:command-unmap-mem-object #x11fd)
+  (:command-marker #x11fe)
+  (:command-acquire-gl-objects #x11ff)
+  (:command-release-gl-objects #x1200)
+  (:command-read-buffer-rect #x1201)
+  (:command-write-buffer-rect #x1202)
+  (:command-copy-buffer-rect #x1203)
+  (:command-user #x1204)
+  (:command-barrier #x1205)
+  (:command-migrate-mem-objects #x1206)
+  (:command-fill-buffer #x1207)
+  (:command-fill-image #x1208)
+  (:command-svm-free #x1209)
+  (:command-svm-memcpy #x120a)
+  (:command-svm-memfill #x120b)
+  (:command-svm-map #x120c)
+  (:command-svm-unmap #x120d)
+  (:command-svm-migrate-mem #x120e))
+
+(defconstant +complete+ #x0)
+(defconstant +running+ #x1)
+(defconstant +submitted+ #x2)
+(defconstant +queued+ #x3)
+
+(cffi:defcenum (cl-buffer-create-type cl-uint)
+    (:buffer-create-type-region #x1220))
+
+(cffi:defcenum (cl-profiling-info cl-uint)
+  (:profiling-command-queued #x1280)
+  (:profiling-command-submit #x1281)
+  (:profiling-command-start #x1282)
+  (:profiling-command-end #x1283)
+  (:profiling-command-complete #x1284))
+
+(cffi:defcenum (cl-khronos-vendor-id cl-uint)
+  (:khronos-vendor-id-codeplay #x10004))
+
+(cffi:defbitfield (cl-device-type cl-bitfield)
+  :device-type-default
+  :device-type-cpu
+  :device-type-gpu
+  :device-type-accelerator
+  :device-type-custom
+  (:device-type-all #xffffffff))
+
+(cffi:defbitfield (cl-device-fp-config cl-bitfield)
+  :fp-denorm
+  :fp-inf-nan
+  :fp-round-to-nearest
+  :fp-round-to-zero
+  :fp-round-to-inf
+  :fp-fma
+  :fp-soft-float
+  :fp-correctly-rounded-divide-sqrt)
+
+(cffi:defbitfield (cl-device-exec-capabilities cl-bitfield)
+  :exec-kernel
+  :exec-native-kernel)
+
+(cffi:defbitfield (cl-device-svm-capabilities cl-bitfield)
+  :device-svm-coarse-grain-buffer
+  :device-svm-fine-grain-buffer
+  :device-svm-fine-grain-system
+  :device-svm-atomics)
+
+(cffi:defbitfield (cl-command-queue-properties cl-bitfield)
+  :queue-out-of-order-exec-mode-enable
+  :queue-profiling-enable
+  :queue-on-device
+  :queue-on-device-default)
+
+(cffi:defbitfield (cl-device-affinity-domain cl-bitfield)
+  :device-affinity-domain-numa
+  :device-affinity-domain-l4-cache
+  :device-affinity-domain-l3-cache
+  :device-affinity-domain-l2-cache
+  :device-affinity-domain-l1-cache
+  :device-affinity-domain-next-partitionable)
+
+(cffi:defbitfield (cl-mem-flags cl-bitfield)
+  :mem-read-write
+  :mem-write-only
+  :mem-read-only
+  :mem-use-host-ptr
+  :mem-alloc-host-ptr
+  :mem-copy-host-ptr
+  (:mem-host-write-only #x80)
+  :mem-host-read-only
+  :mem-host-no-access
+  :mem-svm-fine-grain-buffer
+  :mem-svm-atomics
+  :mem-kernel-read-and-write)
+
+(cffi:defbitfield (cl-svm-mem-flags cl-bitfield)
+  :mem-read-write
+  :mem-write-only
+  :mem-read-only
+  :mem-use-host-ptr
+  :mem-alloc-host-ptr
+  :mem-copy-host-ptr
+  (:mem-host-write-only #x80)
+  :mem-host-read-only
+  :mem-host-no-access
+  :mem-svm-fine-grain-buffer
+  :mem-svm-atomics
+  :mem-kernel-read-and-write)
+
+
+(cffi:defbitfield (cl-mem-migration-flags cl-bitfield)
+  :migrate-mem-object-host
+  :migrate-mem-object-content-undefined)
+
+(cffi:defbitfield (cl-program-binary-type cl-uint)
+  :program-binary-type-none
+  :program-binary-type-compiled-object
+  :program-binary-type-library
+  :program-binary-type-executable)
+
+(cffi:defbitfield (cl-map-flags cl-bitfield)
+  :map-read
+  :map-write
+  :map-write-invalidate-region)
+
+(cffi:defbitfield (cl-kernel-arg-type-qualifier cl-bitfield)
+  (:kernel-arg-type-none+ #x0)
+  :kernel-arg-type-const
+  :kernel-arg-type-restrict
+  :kernel-arg-type-volatile
+  :kernel-arg-type-pipe)
+
+(cffi:defbitfield (cl-device-atomic-capabilities cl-bitfield)
+  :device-atomic-order-relaxed
+  :device-atomic-order-acq-rel
+  :device-atomic-order-seq-cst
+  :device-atomic-scope-work-item
+  :device-atomic-scope-work-group
+  :device-atomic-scope-device
+  :device-atomic-scope-all-devices)
+
+(cffi:defbitfield (cl-device-device-enqueue-capabilities cl-bitfield)
+  :device-queue-supported
+  :device-queue-replaceable-default)
+
+(cffi:defctype cl-mem-properties cl-properties)
+(cffi:defctype cl-queue-properties cl-properties)
+(cffi:defctype cl-device-partition-property :intptr)
+
+(cffi:defcenum (cl-context-properties :intptr :allow-undeclared-values t)
+  (:context-platform #x1084)
+  (:context-interop-user-sync #x1085))
+
+(cffi:defctype cl-pipe-properties :intptr)
+(cffi:defctype cl-sampler-properties cl-properties)
+
+(cffi:defctype cl-version cl-uint)
+
+(cffi:defcstruct cl-image-format
+  (image-channel-order cl-channel-order)
+  (image-channel-data-type cl-channel-type))
+
+(cffi:defcstruct cl-buffer-region
+  (origin :size)
+  (size :size))
+
+(cffi:defcstruct cl-name-version
+  (version cl-version)
+  ;; +name-version-max-name-size+ 64
+  (name :char :count 64))
+
+(cffi:defcstruct cl-image-desc
+  (image-type cl-mem-object-type)
+  (image-width :size)
+  (image-height :size)
+  (image-depth :size)
+  (image-array-size :size)
+  (image-row-pitch :size)
+  (image-slice-pitch :size)
+  (num-mip-levels cl-uint)
+  (num-samples cl-uint)
+  ;; Anon union buffer / mem_object
+  (buffer cl-mem))
author	Thomas Albers <thomas@thomaslabs.org>	2023-03-04 22:47:28 +0100
committer	Thomas Albers <thomas@thomaslabs.org>	2023-03-04 22:47:28 +0100
commit	6fe823a614279cceb2d48507bd8e93b0efd87f94 (patch)
tree	579e3c5db456667ce2aeda94f909703513179ce1 /src