cl

package
v0.0.0-...-aa8867e Latest Latest
Warning

This package is not in the latest version of its module.

Go to latest
Published: Apr 25, 2021 License: BSD-3-Clause Imports: 8 Imported by: 3

Documentation

Overview

Package cl provides a binding to the OpenCL api. It's mostly a low-level wrapper that avoids adding functionality while still making the interface a little more friendly and easy to use.

Resource life-cycle management:

For any CL object that gets created (buffer, queue, kernel, etc..) you should call object.Release() when finished with it to free the CL resources. This explicitely calls the related clXXXRelease method for the type. However, as a fallback there is a finalizer set for every resource item that takes care of it (eventually) if Release isn't called. In this way you can have better control over the life cycle of resources while having a fall back to avoid leaks. This is similar to how file handles and such are handled in the Go standard packages.

Index

Constants

View Source
const (
	ChannelDataTypeUNormInt24  ChannelDataType = C.CL_UNORM_INT24
	ChannelOrderDepth          ChannelOrder    = C.CL_DEPTH
	ChannelOrderDepthStencil   ChannelOrder    = C.CL_DEPTH_STENCIL
	MemHostNoAccess            MemFlag         = C.CL_MEM_HOST_NO_ACCESS  // OpenCL 1.2
	MemHostReadOnly            MemFlag         = C.CL_MEM_HOST_READ_ONLY  // OpenCL 1.2
	MemHostWriteOnly           MemFlag         = C.CL_MEM_HOST_WRITE_ONLY // OpenCL 1.2
	MemObjectTypeImage1D       MemObjectType   = C.CL_MEM_OBJECT_IMAGE1D
	MemObjectTypeImage1DArray  MemObjectType   = C.CL_MEM_OBJECT_IMAGE1D_ARRAY
	MemObjectTypeImage1DBuffer MemObjectType   = C.CL_MEM_OBJECT_IMAGE1D_BUFFER
	MemObjectTypeImage2DArray  MemObjectType   = C.CL_MEM_OBJECT_IMAGE2D_ARRAY
	// MapFlagWriteInvalidateRegion specifies that the region being mapped in the memory object is being mapped for writing.
	//
	// The contents of the region being mapped are to be discarded. This is typically the case when the
	// region being mapped is overwritten by the host. This flag allows the implementation to no longer
	// guarantee that the pointer returned by clEnqueueMapBuffer or clEnqueueMapImage contains the
	// latest bits in the region being mapped which can be a significant performance enhancement.
	MapFlagWriteInvalidateRegion MapFlag = C.CL_MAP_WRITE_INVALIDATE_REGION
)

Variables

View Source
var (
	ErrDeviceNotFound                     = errors.New("cl: Device Not Found")
	ErrDeviceNotAvailable                 = errors.New("cl: Device Not Available")
	ErrCompilerNotAvailable               = errors.New("cl: Compiler Not Available")
	ErrMemObjectAllocationFailure         = errors.New("cl: Mem Object Allocation Failure")
	ErrOutOfResources                     = errors.New("cl: Out Of Resources")
	ErrOutOfHostMemory                    = errors.New("cl: Out Of Host Memory")
	ErrProfilingInfoNotAvailable          = errors.New("cl: Profiling Info Not Available")
	ErrMemCopyOverlap                     = errors.New("cl: Mem Copy Overlap")
	ErrImageFormatMismatch                = errors.New("cl: Image Format Mismatch")
	ErrImageFormatNotSupported            = errors.New("cl: Image Format Not Supported")
	ErrBuildProgramFailure                = errors.New("cl: Build Program Failure")
	ErrMapFailure                         = errors.New("cl: Map Failure")
	ErrMisalignedSubBufferOffset          = errors.New("cl: Misaligned Sub Buffer Offset")
	ErrExecStatusErrorForEventsInWaitList = errors.New("cl: Exec Status Error For Events In Wait List")
	ErrCompileProgramFailure              = errors.New("cl: Compile Program Failure")
	ErrLinkerNotAvailable                 = errors.New("cl: Linker Not Available")
	ErrLinkProgramFailure                 = errors.New("cl: Link Program Failure")
	ErrDevicePartitionFailed              = errors.New("cl: Device Partition Failed")
	ErrKernelArgInfoNotAvailable          = errors.New("cl: Kernel Arg Info Not Available")
	ErrInvalidValue                       = errors.New("cl: Invalid Value")
	ErrInvalidDeviceType                  = errors.New("cl: Invalid Device Type")
	ErrInvalidPlatform                    = errors.New("cl: Invalid Platform")
	ErrInvalidDevice                      = errors.New("cl: Invalid Device")
	ErrInvalidContext                     = errors.New("cl: Invalid Context")
	ErrInvalidQueueProperties             = errors.New("cl: Invalid Queue Properties")
	ErrInvalidCommandQueue                = errors.New("cl: Invalid Command Queue")
	ErrInvalidHostPtr                     = errors.New("cl: Invalid Host Ptr")
	ErrInvalidMemObject                   = errors.New("cl: Invalid Mem Object")
	ErrInvalidImageFormatDescriptor       = errors.New("cl: Invalid Image Format Descriptor")
	ErrInvalidImageSize                   = errors.New("cl: Invalid Image Size")
	ErrInvalidSampler                     = errors.New("cl: Invalid Sampler")
	ErrInvalidBinary                      = errors.New("cl: Invalid Binary")
	ErrInvalidBuildOptions                = errors.New("cl: Invalid Build Options")
	ErrInvalidProgram                     = errors.New("cl: Invalid Program")
	ErrInvalidProgramExecutable           = errors.New("cl: Invalid Program Executable")
	ErrInvalidKernelName                  = errors.New("cl: Invalid Kernel Name")
	ErrInvalidKernelDefinition            = errors.New("cl: Invalid Kernel Definition")
	ErrInvalidKernel                      = errors.New("cl: Invalid Kernel")
	ErrInvalidArgIndex                    = errors.New("cl: Invalid Arg Index")
	ErrInvalidArgValue                    = errors.New("cl: Invalid Arg Value")
	ErrInvalidArgSize                     = errors.New("cl: Invalid Arg Size")
	ErrInvalidKernelArgs                  = errors.New("cl: Invalid Kernel Args")
	ErrInvalidWorkDimension               = errors.New("cl: Invalid Work Dimension")
	ErrInvalidWorkGroupSize               = errors.New("cl: Invalid Work Group Size")
	ErrInvalidWorkItemSize                = errors.New("cl: Invalid Work Item Size")
	ErrInvalidGlobalOffset                = errors.New("cl: Invalid Global Offset")
	ErrInvalidEventWaitList               = errors.New("cl: Invalid Event Wait List")
	ErrInvalidEvent                       = errors.New("cl: Invalid Event")
	ErrInvalidOperation                   = errors.New("cl: Invalid Operation")
	ErrInvalidGlObject                    = errors.New("cl: Invalid Gl Object")
	ErrInvalidBufferSize                  = errors.New("cl: Invalid Buffer Size")
	ErrInvalidMipLevel                    = errors.New("cl: Invalid Mip Level")
	ErrInvalidGlobalWorkSize              = errors.New("cl: Invalid Global Work Size")
	ErrInvalidProperty                    = errors.New("cl: Invalid Property")
	ErrInvalidImageDescriptor             = errors.New("cl: Invalid Image Descriptor")
	ErrInvalidCompilerOptions             = errors.New("cl: Invalid Compiler Options")
	ErrInvalidLinkerOptions               = errors.New("cl: Invalid Linker Options")
	ErrInvalidDevicePartitionCount        = errors.New("cl: Invalid Device Partition Count")
)
View Source
var (
	ErrUnknown = errors.New("cl: unknown error") // Generally an unexpected result from an OpenCL function (e.g. CL_SUCCESS but null pointer)
)
View Source
var ErrUnsupported = errors.New("cl: unsupported")

ErrUnsupported is the error returned when some functionality is not supported

Functions

func WaitForEvents

func WaitForEvents(events []*Event) error

WaitForEvents waits on the host thread for commands identified by event objects in events to complete. A command is considered complete if its execution status is CL_COMPLETE or a negative value. The events specified in event_list act as synchronization points.

If the cl_khr_gl_event extension is enabled, event objects can also be used to reflect the status of an OpenGL sync object. The sync object in turn refers to a fence command executing in an OpenGL command stream. This provides another method of coordinating sharing of buffers and images between OpenGL and OpenCL.

Types

type BuildError

type BuildError string

func (BuildError) Error

func (e BuildError) Error() string

type ChannelDataType

type ChannelDataType int
const (
	ChannelDataTypeSNormInt8      ChannelDataType = C.CL_SNORM_INT8
	ChannelDataTypeSNormInt16     ChannelDataType = C.CL_SNORM_INT16
	ChannelDataTypeUNormInt8      ChannelDataType = C.CL_UNORM_INT8
	ChannelDataTypeUNormInt16     ChannelDataType = C.CL_UNORM_INT16
	ChannelDataTypeUNormShort565  ChannelDataType = C.CL_UNORM_SHORT_565
	ChannelDataTypeUNormShort555  ChannelDataType = C.CL_UNORM_SHORT_555
	ChannelDataTypeUNormInt101010 ChannelDataType = C.CL_UNORM_INT_101010
	ChannelDataTypeSignedInt8     ChannelDataType = C.CL_SIGNED_INT8
	ChannelDataTypeSignedInt16    ChannelDataType = C.CL_SIGNED_INT16
	ChannelDataTypeSignedInt32    ChannelDataType = C.CL_SIGNED_INT32
	ChannelDataTypeUnsignedInt8   ChannelDataType = C.CL_UNSIGNED_INT8
	ChannelDataTypeUnsignedInt16  ChannelDataType = C.CL_UNSIGNED_INT16
	ChannelDataTypeUnsignedInt32  ChannelDataType = C.CL_UNSIGNED_INT32
	ChannelDataTypeHalfFloat      ChannelDataType = C.CL_HALF_FLOAT
	ChannelDataTypeFloat          ChannelDataType = C.CL_FLOAT
)

func (ChannelDataType) String

func (ct ChannelDataType) String() string

type ChannelOrder

type ChannelOrder int
const (
	ChannelOrderR         ChannelOrder = C.CL_R
	ChannelOrderA         ChannelOrder = C.CL_A
	ChannelOrderRG        ChannelOrder = C.CL_RG
	ChannelOrderRA        ChannelOrder = C.CL_RA
	ChannelOrderRGB       ChannelOrder = C.CL_RGB
	ChannelOrderRGBA      ChannelOrder = C.CL_RGBA
	ChannelOrderBGRA      ChannelOrder = C.CL_BGRA
	ChannelOrderARGB      ChannelOrder = C.CL_ARGB
	ChannelOrderIntensity ChannelOrder = C.CL_INTENSITY
	ChannelOrderLuminance ChannelOrder = C.CL_LUMINANCE
	ChannelOrderRx        ChannelOrder = C.CL_Rx
	ChannelOrderRGx       ChannelOrder = C.CL_RGx
	ChannelOrderRGBx      ChannelOrder = C.CL_RGBx
)

func (ChannelOrder) String

func (co ChannelOrder) String() string

type CommandExecStatus

type CommandExecStatus int
const (
	CommandExecStatusComplete  CommandExecStatus = C.CL_COMPLETE
	CommandExecStatusRunning   CommandExecStatus = C.CL_RUNNING
	CommandExecStatusSubmitted CommandExecStatus = C.CL_SUBMITTED
	CommandExecStatusQueued    CommandExecStatus = C.CL_QUEUED
)

type CommandQueue

type CommandQueue struct {
	// contains filtered or unexported fields
}

func (*CommandQueue) EnqueueBarrierWithWaitList

func (q *CommandQueue) EnqueueBarrierWithWaitList(eventWaitList []*Event) (*Event, error)

EnqueueBarrierWithWaitList enqueues a synchronization point that enqueues a barrier operation.

func (*CommandQueue) EnqueueCopyBuffer

func (q *CommandQueue) EnqueueCopyBuffer(srcBuffer, dstBuffer *MemObject, srcOffset, dstOffset, byteCount int, eventWaitList []*Event) (*Event, error)

EnqueueCopyBuffer enqueues a command to copy a buffer object to another buffer object.

func (*CommandQueue) EnqueueFillBuffer

func (q *CommandQueue) EnqueueFillBuffer(buffer *MemObject, pattern unsafe.Pointer, patternSize, offset, size int, eventWaitList []*Event) (*Event, error)

EnqueueFillBuffer enqueues a command to fill a buffer object with a pattern of a given pattern size.

func (*CommandQueue) EnqueueMapBuffer

func (q *CommandQueue) EnqueueMapBuffer(buffer *MemObject, blocking bool, flags MapFlag, offset, size int, eventWaitList []*Event) (*MappedMemObject, *Event, error)

EnqueueMapBuffer enqueues a command to map a region of the buffer object given by buffer into the host address space and returns a pointer to this mapped region.

func (*CommandQueue) EnqueueMapImage

func (q *CommandQueue) EnqueueMapImage(buffer *MemObject, blocking bool, flags MapFlag, origin, region [3]int, eventWaitList []*Event) (*MappedMemObject, *Event, error)

EnqueueMapImage enqueues a command to map a region of an image object into the host address space and returns a pointer to this mapped region.

func (*CommandQueue) EnqueueMarkerWithWaitList

func (q *CommandQueue) EnqueueMarkerWithWaitList(eventWaitList []*Event) (*Event, error)

EnqueueMarkerWithWaitList enqueues a marker command which waits for either a list of events to complete, or all previously enqueued commands to complete.

func (*CommandQueue) EnqueueNDRangeKernel

func (q *CommandQueue) EnqueueNDRangeKernel(kernel *Kernel, globalWorkOffset, globalWorkSize, localWorkSize []int, eventWaitList []*Event) (*Event, error)

EnqueueNDRangeKernel enqueues a command to execute a kernel on a device.

func (*CommandQueue) EnqueueReadBuffer

func (q *CommandQueue) EnqueueReadBuffer(buffer *MemObject, blocking bool, offset, dataSize int, dataPtr unsafe.Pointer, eventWaitList []*Event) (*Event, error)

EnqueueReadBuffer enqueues commands to read from a buffer object to host memory.

func (*CommandQueue) EnqueueReadBufferFloat32

func (q *CommandQueue) EnqueueReadBufferFloat32(buffer *MemObject, blocking bool, offset int, data []float32, eventWaitList []*Event) (*Event, error)

func (*CommandQueue) EnqueueReadImage

func (q *CommandQueue) EnqueueReadImage(image *MemObject, blocking bool, origin, region [3]int, rowPitch, slicePitch int, data []byte, eventWaitList []*Event) (*Event, error)

EnqueueReadImage enqueues a command to read from a 2D or 3D image object to host memory.

func (*CommandQueue) EnqueueTask

func (q *CommandQueue) EnqueueTask(kernel *Kernel, eventWaitList []*Event) (*Event, error)

EnqueueTask enqueues a task to execute a kernel on a device. The kernel is executed using a single work-item. EnqueueTask is equivalent to calling EnqueueNDRangeKernel with globalWorkOffset = 0, globalWorkSize[0] set to 1, and localWorkSize[0] set to 1.

func (*CommandQueue) EnqueueUnmapMemObject

func (q *CommandQueue) EnqueueUnmapMemObject(buffer *MemObject, mappedObj *MappedMemObject, eventWaitList []*Event) (*Event, error)

EnqueueUnmapMemObject enqueues a command to unmap a previously mapped region of a memory object.

func (*CommandQueue) EnqueueWriteBuffer

func (q *CommandQueue) EnqueueWriteBuffer(buffer *MemObject, blocking bool, offset, dataSize int, dataPtr unsafe.Pointer, eventWaitList []*Event) (*Event, error)

EnqueueWriteBuffer enqueues commands to write to a buffer object from host memory.

func (*CommandQueue) EnqueueWriteBufferFloat32

func (q *CommandQueue) EnqueueWriteBufferFloat32(buffer *MemObject, blocking bool, offset int, data []float32, eventWaitList []*Event) (*Event, error)

func (*CommandQueue) EnqueueWriteImage

func (q *CommandQueue) EnqueueWriteImage(image *MemObject, blocking bool, origin, region [3]int, rowPitch, slicePitch int, data []byte, eventWaitList []*Event) (*Event, error)

EnqueueWriteImage enqueues a command to write from a 2D or 3D image object to host memory.

func (*CommandQueue) Finish

func (q *CommandQueue) Finish() error

Finish blocks until all previously queued OpenCL commands in a command-queue are issued to the associated device and have completed.

func (*CommandQueue) Flush

func (q *CommandQueue) Flush() error

Flush issues all previously queued OpenCL commands in a command-queue to the device associated with the command-queue.

func (*CommandQueue) Release

func (q *CommandQueue) Release()

Release calls clReleaseCommandQueue on the CommandQueue. Using the CommandQueue after Release will cause a panick.

type CommandQueueProperty

type CommandQueueProperty int
const (
	CommandQueueOutOfOrderExecModeEnable CommandQueueProperty = C.CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE
	CommandQueueProfilingEnable          CommandQueueProperty = C.CL_QUEUE_PROFILING_ENABLE
)

type Context

type Context struct {
	// contains filtered or unexported fields
}

func CreateContext

func CreateContext(devices []*Device) (*Context, error)

TODO: properties

func (*Context) CreateBuffer

func (ctx *Context) CreateBuffer(flags MemFlag, data []byte) (*MemObject, error)

func (*Context) CreateBufferFloat32

func (ctx *Context) CreateBufferFloat32(flags MemFlag, data []float32) (*MemObject, error)

func (*Context) CreateBufferUnsafe

func (ctx *Context) CreateBufferUnsafe(flags MemFlag, size int, dataPtr unsafe.Pointer) (*MemObject, error)

func (*Context) CreateCommandQueue

func (ctx *Context) CreateCommandQueue(device *Device, properties CommandQueueProperty) (*CommandQueue, error)

func (*Context) CreateEmptyBuffer

func (ctx *Context) CreateEmptyBuffer(flags MemFlag, size int) (*MemObject, error)

func (*Context) CreateImage

func (ctx *Context) CreateImage(flags MemFlag, imageFormat ImageFormat, imageDesc ImageDescription, data []byte) (*MemObject, error)

func (*Context) CreateImageFromImage

func (ctx *Context) CreateImageFromImage(flags MemFlag, img image.Image) (*MemObject, error)

func (*Context) CreateImageSimple

func (ctx *Context) CreateImageSimple(flags MemFlag, width, height int, channelOrder ChannelOrder, channelDataType ChannelDataType, data []byte) (*MemObject, error)

func (*Context) CreateProgramWithSource

func (ctx *Context) CreateProgramWithSource(sources []string) (*Program, error)

func (*Context) CreateUserEvent

func (ctx *Context) CreateUserEvent() (*Event, error)

func (*Context) GetSupportedImageFormats

func (ctx *Context) GetSupportedImageFormats(flags MemFlag, imageType MemObjectType) ([]ImageFormat, error)

func (*Context) Release

func (ctx *Context) Release()

type Device

type Device struct {
	// contains filtered or unexported fields
}

func GetDevices

func GetDevices(platform *Platform, deviceType DeviceType) ([]*Device, error)

Obtain the list of devices available on a platform. 'platform' refers to the platform returned by GetPlatforms or can be nil. If platform is nil, the behavior is implementation-defined.

func (*Device) AddressBits

func (d *Device) AddressBits() int

The default compute device address space size specified as an unsigned integer value in bits. Currently supported values are 32 or 64 bits.

func (*Device) Available

func (d *Device) Available() bool

func (*Device) BuiltInKernels

func (d *Device) BuiltInKernels() string

func (*Device) CompilerAvailable

func (d *Device) CompilerAvailable() bool

func (*Device) DoubleFPConfig

func (d *Device) DoubleFPConfig() FPConfig

DoubleFPConfig describes double precision floating-point capability of the OpenCL device

func (*Device) DriverVersion

func (d *Device) DriverVersion() string

func (*Device) EndianLittle

func (d *Device) EndianLittle() bool

func (*Device) ErrorCorrectionSupport

func (d *Device) ErrorCorrectionSupport() bool

Is CL_TRUE if the device implements error correction for all accesses to compute device memory (global and constant). Is CL_FALSE if the device does not implement such error correction.

func (*Device) ExecutionCapabilities

func (d *Device) ExecutionCapabilities() ExecCapability

ExecutionCapabilities describes the execution capabilities of the device. The mandated minimum capability is CL_EXEC_KERNEL.

func (*Device) Extensions

func (d *Device) Extensions() string

func (*Device) GetInfoBool

func (d *Device) GetInfoBool(param C.cl_device_info) (bool, error)

func (*Device) GetInfoSize

func (d *Device) GetInfoSize(param C.cl_device_info) (int, error)

func (*Device) GetInfoString

func (d *Device) GetInfoString(param C.cl_device_info) (string, error)

func (*Device) GetInfoUint

func (d *Device) GetInfoUint(param C.cl_device_info) (uint, error)

func (*Device) GetInfoUlong

func (d *Device) GetInfoUlong(param C.cl_device_info) (int64, error)

func (*Device) GlobalMemCacheSize

func (d *Device) GlobalMemCacheSize() int

func (*Device) GlobalMemCacheType

func (d *Device) GlobalMemCacheType() MemCacheType

func (*Device) GlobalMemCachelineSize

func (d *Device) GlobalMemCachelineSize() int

Size of global memory cache line in bytes.

func (*Device) GlobalMemSize

func (d *Device) GlobalMemSize() int64

Size of global device memory in bytes.

func (*Device) HalfFPConfig

func (d *Device) HalfFPConfig() FPConfig

HalfFPConfig describes the OPTIONAL half precision floating-point capability of the OpenCL device

func (*Device) HostUnifiedMemory

func (d *Device) HostUnifiedMemory() bool

func (*Device) Image2DMaxHeight

func (d *Device) Image2DMaxHeight() int

Image2DMaxHeight returns the max height of 2D image in pixels. The minimum value is 8192 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE.

func (*Device) Image2DMaxWidth

func (d *Device) Image2DMaxWidth() int

Image2DMaxWidth returns the max width of 2D image or 1D image not created from a buffer object in pixels. The minimum value is 8192 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE.

func (*Device) Image3DMaxDepth

func (d *Device) Image3DMaxDepth() int

Image3DMaxDepth returns the max depth of 3D image in pixels. The minimum value is 2048 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE.

func (*Device) Image3DMaxHeight

func (d *Device) Image3DMaxHeight() int

Image3DMaxHeight returns the max height of 3D image in pixels. The minimum value is 2048 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE.

func (*Device) Image3DMaxWidth

func (d *Device) Image3DMaxWidth() int

Image3DMaxWidth returns the max width of 3D image in pixels. The minimum value is 2048 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE.

func (*Device) ImageMaxArraySize

func (d *Device) ImageMaxArraySize() int

Max number of images in a 1D or 2D image array. The minimum value is 2048 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE

func (*Device) ImageMaxBufferSize

func (d *Device) ImageMaxBufferSize() int

Max number of pixels for a 1D image created from a buffer object. The minimum value is 65536 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE.

func (*Device) ImageSupport

func (d *Device) ImageSupport() bool

func (*Device) LinkerAvailable

func (d *Device) LinkerAvailable() bool

Is CL_FALSE if the implementation does not have a linker available. Is CL_TRUE if the linker is available. This can be CL_FALSE for the embedded platform profile only. This must be CL_TRUE if CL_DEVICE_COMPILER_AVAILABLE is CL_TRUE

func (*Device) LocalMemSize

func (d *Device) LocalMemSize() int64

LocalMemSize returns the size of local memory arena in bytes. The minimum value is 32 KB for devices that are not of type CL_DEVICE_TYPE_CUSTOM.

func (*Device) LocalMemType

func (d *Device) LocalMemType() LocalMemType

LocalMemType returns the type of local memory supported. This can be set to CL_LOCAL implying dedicated local memory storage such as SRAM, or CL_GLOBAL. For custom devices, CL_NONE can also be returned indicating no local memory support.

func (*Device) MaxClockFrequency

func (d *Device) MaxClockFrequency() int

Maximum configured clock frequency of the device in MHz.

func (*Device) MaxComputeUnits

func (d *Device) MaxComputeUnits() int

MaxComputeUnits returns the number of parallel compute units on the OpenCL device. A work-group executes on a single compute unit. The minimum value is 1.

func (*Device) MaxConstantArgs

func (d *Device) MaxConstantArgs() int

MaxConstantArgs returns the max number of arguments declared with the __constant qualifier in a kernel. The minimum value is 8 for devices that are not of type CL_DEVICE_TYPE_CUSTOM.

func (*Device) MaxConstantBufferSize

func (d *Device) MaxConstantBufferSize() int64

MaxConstantBufferSize returns the max size in bytes of a constant buffer allocation. The minimum value is 64 KB for devices that are not of type CL_DEVICE_TYPE_CUSTOM.

func (*Device) MaxMemAllocSize

func (d *Device) MaxMemAllocSize() int64

MaxMemAllocSize returns the max size of memory object allocation in bytes. The minimum value is max (1/4th of CL_DEVICE_GLOBAL_MEM_SIZE, 128*1024*1024) for devices that are not of type CL_DEVICE_TYPE_CUSTOM.

func (*Device) MaxParameterSize

func (d *Device) MaxParameterSize() int

MaxParameterSize returns the max size in bytes of the arguments that can be passed to a kernel. The minimum value is 1024 for devices that are not of type CL_DEVICE_TYPE_CUSTOM. For this minimum value, only a maximum of 128 arguments can be passed to a kernel.

func (*Device) MaxReadImageArgs

func (d *Device) MaxReadImageArgs() int

MaxReadImageArgs returns the max number of simultaneous image objects that can be read by a kernel. The minimum value is 128 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE.

func (*Device) MaxSamplers

func (d *Device) MaxSamplers() int

MaxSamplers returns the maximum number of samplers that can be used in a kernel. The minimum value is 16 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE. (Also see sampler_t.)

func (*Device) MaxWorkGroupSize

func (d *Device) MaxWorkGroupSize() int

MaxWorkGroupSize returns the maximum number of work-items in a work-group executing a kernel on a single compute unit, using the data parallel execution model. (Refer to clEnqueueNDRangeKernel). The minimum value is 1.

func (*Device) MaxWorkItemDimensions

func (d *Device) MaxWorkItemDimensions() int

MaxWorkItemDimensions returns the maximum dimensions that specify the global and local work-item IDs used by the data parallel execution model. (Refer to clEnqueueNDRangeKernel). The minimum value is 3 for devices that are not of type CL_DEVICE_TYPE_CUSTOM.

func (*Device) MaxWorkItemSizes

func (d *Device) MaxWorkItemSizes() []int

MaxWorkItemSizes returns the maximum number of work-items that can be specified in each dimension of the work-group to clEnqueueNDRangeKernel.

Returns n size_t entries, where n is the value returned by the query for CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS.

The minimum value is (1, 1, 1) for devices that are not of type CL_DEVICE_TYPE_CUSTOM.

func (*Device) MaxWriteImageArgs

func (d *Device) MaxWriteImageArgs() int

MaxWriteImageArgs returns the max number of simultaneous image objects that can be written to by a kernel. The minimum value is 8 if CL_DEVICE_IMAGE_SUPPORT is CL_TRUE.

func (*Device) MemBaseAddrAlign

func (d *Device) MemBaseAddrAlign() int

The minimum value is the size (in bits) of the largest OpenCL built-in data type supported by the device (long16 in FULL profile, long16 or int16 in EMBEDDED profile) for devices that are not of type CL_DEVICE_TYPE_CUSTOM.

func (*Device) Name

func (d *Device) Name() string

func (*Device) NativeVectorWidthChar

func (d *Device) NativeVectorWidthChar() int

func (*Device) NativeVectorWidthDouble

func (d *Device) NativeVectorWidthDouble() int

func (*Device) NativeVectorWidthFloat

func (d *Device) NativeVectorWidthFloat() int

func (*Device) NativeVectorWidthHalf

func (d *Device) NativeVectorWidthHalf() int

func (*Device) NativeVectorWidthInt

func (d *Device) NativeVectorWidthInt() int

func (*Device) NativeVectorWidthLong

func (d *Device) NativeVectorWidthLong() int

func (*Device) NativeVectorWidthShort

func (d *Device) NativeVectorWidthShort() int

func (*Device) OpenCLCVersion

func (d *Device) OpenCLCVersion() string

func (*Device) ParentDevice

func (d *Device) ParentDevice() *Device

func (*Device) PreferredVectorWidthChar

func (d *Device) PreferredVectorWidthChar() int

func (*Device) PreferredVectorWidthDouble

func (d *Device) PreferredVectorWidthDouble() int

func (*Device) PreferredVectorWidthFloat

func (d *Device) PreferredVectorWidthFloat() int

func (*Device) PreferredVectorWidthHalf

func (d *Device) PreferredVectorWidthHalf() int

func (*Device) PreferredVectorWidthInt

func (d *Device) PreferredVectorWidthInt() int

func (*Device) PreferredVectorWidthLong

func (d *Device) PreferredVectorWidthLong() int

func (*Device) PreferredVectorWidthShort

func (d *Device) PreferredVectorWidthShort() int

func (*Device) Profile

func (d *Device) Profile() string

func (*Device) ProfilingTimerResolution

func (d *Device) ProfilingTimerResolution() int

ProfilingTimerResolution describes the resolution of device timer. This is measured in nanoseconds.

func (*Device) Type

func (d *Device) Type() DeviceType

func (*Device) Vendor

func (d *Device) Vendor() string

func (*Device) Version

func (d *Device) Version() string

type DeviceType

type DeviceType uint
const (
	DeviceTypeCPU         DeviceType = C.CL_DEVICE_TYPE_CPU
	DeviceTypeGPU         DeviceType = C.CL_DEVICE_TYPE_GPU
	DeviceTypeAccelerator DeviceType = C.CL_DEVICE_TYPE_ACCELERATOR
	DeviceTypeDefault     DeviceType = C.CL_DEVICE_TYPE_DEFAULT
	DeviceTypeAll         DeviceType = C.CL_DEVICE_TYPE_ALL
)

func (DeviceType) String

func (dt DeviceType) String() string

type ErrOther

type ErrOther int

func (ErrOther) Error

func (e ErrOther) Error() string

type ErrUnsupportedArgumentType

type ErrUnsupportedArgumentType struct {
	Index int
	Value interface{}
}

func (ErrUnsupportedArgumentType) Error

type Event

type Event struct {
	// contains filtered or unexported fields
}

func (*Event) GetEventProfilingInfo

func (e *Event) GetEventProfilingInfo(paramName ProfilingInfo) (int64, error)

func (*Event) GetExecutionStatus

func (e *Event) GetExecutionStatus() (CommandExecStatus, error)

func (*Event) Release

func (e *Event) Release()

func (*Event) SetUserEventStatus

func (e *Event) SetUserEventStatus(status int) error

SetUserEventStatus sets the execution status of a user event object.

`status` specifies the new execution status to be set and can be CL_COMPLETE or a negative integer value to indicate an error. A negative integer value causes all enqueued commands that wait on this user event to be terminated. clSetUserEventStatus can only be called once to change the execution status of event.

type ExecCapability

type ExecCapability int
const (
	ExecCapabilityKernel       ExecCapability = C.CL_EXEC_KERNEL        // The OpenCL device can execute OpenCL kernels.
	ExecCapabilityNativeKernel ExecCapability = C.CL_EXEC_NATIVE_KERNEL // The OpenCL device can execute native kernels.
)

func (ExecCapability) String

func (ec ExecCapability) String() string

type FPConfig

type FPConfig int
const (
	FPConfigDenorm         FPConfig = C.CL_FP_DENORM           // denorms are supported
	FPConfigInfNaN         FPConfig = C.CL_FP_INF_NAN          // INF and NaNs are supported
	FPConfigRoundToNearest FPConfig = C.CL_FP_ROUND_TO_NEAREST // round to nearest even rounding mode supported
	FPConfigRoundToZero    FPConfig = C.CL_FP_ROUND_TO_ZERO    // round to zero rounding mode supported
	FPConfigRoundToInf     FPConfig = C.CL_FP_ROUND_TO_INF     // round to positive and negative infinity rounding modes supported
	FPConfigFMA            FPConfig = C.CL_FP_FMA              // IEEE754-2008 fused multiply-add is supported
	FPConfigSoftFloat      FPConfig = C.CL_FP_SOFT_FLOAT       // Basic floating-point operations (such as addition, subtraction, multiplication) are implemented in software
)
const FPConfigCorrectlyRoundedDivideSqrt FPConfig = C.CL_FP_CORRECTLY_ROUNDED_DIVIDE_SQRT

func (FPConfig) String

func (c FPConfig) String() string

type ImageDescription

type ImageDescription struct {
	Type                            MemObjectType
	Width, Height, Depth            int
	ArraySize, RowPitch, SlicePitch int
	NumMipLevels, NumSamples        int
	Buffer                          *MemObject
}

type ImageFormat

type ImageFormat struct {
	ChannelOrder    ChannelOrder
	ChannelDataType ChannelDataType
}

type Kernel

type Kernel struct {
	// contains filtered or unexported fields
}

func (*Kernel) ArgName

func (k *Kernel) ArgName(index int) (string, error)

func (*Kernel) NumArgs

func (k *Kernel) NumArgs() (int, error)

func (*Kernel) PreferredWorkGroupSizeMultiple

func (k *Kernel) PreferredWorkGroupSizeMultiple(device *Device) (int, error)

func (*Kernel) Release

func (k *Kernel) Release()

func (*Kernel) SetArg

func (k *Kernel) SetArg(index int, arg interface{}) error

func (*Kernel) SetArgBuffer

func (k *Kernel) SetArgBuffer(index int, buffer *MemObject) error

func (*Kernel) SetArgFloat32

func (k *Kernel) SetArgFloat32(index int, val float32) error

func (*Kernel) SetArgInt32

func (k *Kernel) SetArgInt32(index int, val int32) error

func (*Kernel) SetArgInt64

func (k *Kernel) SetArgInt64(index int, val int64) error

func (*Kernel) SetArgInt8

func (k *Kernel) SetArgInt8(index int, val int8) error

func (*Kernel) SetArgLocal

func (k *Kernel) SetArgLocal(index int, size int) error

func (*Kernel) SetArgUint32

func (k *Kernel) SetArgUint32(index int, val uint32) error

func (*Kernel) SetArgUint64

func (k *Kernel) SetArgUint64(index int, val uint64) error

func (*Kernel) SetArgUint8

func (k *Kernel) SetArgUint8(index int, val uint8) error

func (*Kernel) SetArgUnsafe

func (k *Kernel) SetArgUnsafe(index, argSize int, arg unsafe.Pointer) error

func (*Kernel) SetArgs

func (k *Kernel) SetArgs(args ...interface{}) error

func (*Kernel) WorkGroupSize

func (k *Kernel) WorkGroupSize(device *Device) (int, error)

type LocalBuffer

type LocalBuffer int

type LocalMemType

type LocalMemType int
const (
	LocalMemTypeNone   LocalMemType = C.CL_NONE
	LocalMemTypeGlobal LocalMemType = C.CL_GLOBAL
	LocalMemTypeLocal  LocalMemType = C.CL_LOCAL
)

func (LocalMemType) String

func (t LocalMemType) String() string

type MapFlag

type MapFlag int
const (
	// This flag specifies that the region being mapped in the memory object is being mapped for reading.
	MapFlagRead  MapFlag = C.CL_MAP_READ
	MapFlagWrite MapFlag = C.CL_MAP_WRITE
)

type MappedMemObject

type MappedMemObject struct {
	// contains filtered or unexported fields
}

func (*MappedMemObject) ByteSlice

func (mb *MappedMemObject) ByteSlice() []byte

func (*MappedMemObject) Ptr

func (mb *MappedMemObject) Ptr() unsafe.Pointer

func (*MappedMemObject) RowPitch

func (mb *MappedMemObject) RowPitch() int

func (*MappedMemObject) Size

func (mb *MappedMemObject) Size() int

func (*MappedMemObject) SlicePitch

func (mb *MappedMemObject) SlicePitch() int

type MemCacheType

type MemCacheType int
const (
	MemCacheTypeNone           MemCacheType = C.CL_NONE
	MemCacheTypeReadOnlyCache  MemCacheType = C.CL_READ_ONLY_CACHE
	MemCacheTypeReadWriteCache MemCacheType = C.CL_READ_WRITE_CACHE
)

func (MemCacheType) String

func (ct MemCacheType) String() string

type MemFlag

type MemFlag int
const (
	MemReadWrite    MemFlag = C.CL_MEM_READ_WRITE
	MemWriteOnly    MemFlag = C.CL_MEM_WRITE_ONLY
	MemReadOnly     MemFlag = C.CL_MEM_READ_ONLY
	MemUseHostPtr   MemFlag = C.CL_MEM_USE_HOST_PTR
	MemAllocHostPtr MemFlag = C.CL_MEM_ALLOC_HOST_PTR
	MemCopyHostPtr  MemFlag = C.CL_MEM_COPY_HOST_PTR
)

type MemObject

type MemObject struct {
	// contains filtered or unexported fields
}

func (*MemObject) Release

func (b *MemObject) Release()

type MemObjectType

type MemObjectType int
const (
	MemObjectTypeBuffer  MemObjectType = C.CL_MEM_OBJECT_BUFFER
	MemObjectTypeImage2D MemObjectType = C.CL_MEM_OBJECT_IMAGE2D
	MemObjectTypeImage3D MemObjectType = C.CL_MEM_OBJECT_IMAGE3D
)

type Platform

type Platform struct {
	// contains filtered or unexported fields
}

func GetPlatforms

func GetPlatforms() ([]*Platform, error)

Obtain the list of platforms available.

func (*Platform) Extensions

func (p *Platform) Extensions() string

func (*Platform) GetDevices

func (p *Platform) GetDevices(deviceType DeviceType) ([]*Device, error)

func (*Platform) Name

func (p *Platform) Name() string

func (*Platform) Profile

func (p *Platform) Profile() string

func (*Platform) Vendor

func (p *Platform) Vendor() string

func (*Platform) Version

func (p *Platform) Version() string

type ProfilingInfo

type ProfilingInfo int
const (
	// ProfilingInfoCommandQueued is a 64-bit value that describes the current device time counter in
	// nanoseconds when the command identified by event is enqueued in
	// a command-queue by the host.
	ProfilingInfoCommandQueued ProfilingInfo = C.CL_PROFILING_COMMAND_QUEUED
	// ProfilingInfoCommandSubmit is a 64-bit value that describes the current device time counter in
	// nanoseconds when the command identified by event that has been
	// enqueued is submitted by the host to the device associated with the command-queue.
	ProfilingInfoCommandSubmit ProfilingInfo = C.CL_PROFILING_COMMAND_SUBMIT
	// ProfilingInfoCommandStart is a 64-bit value that describes the current device time counter in
	// nanoseconds when the command identified by event starts execution on the device.
	ProfilingInfoCommandStart ProfilingInfo = C.CL_PROFILING_COMMAND_START
	// ProfilingInfoCommandEnd is a 64-bit value that describes the current device time counter in
	// nanoseconds when the command identified by event has finished
	// execution on the device.
	ProfilingInfoCommandEnd ProfilingInfo = C.CL_PROFILING_COMMAND_END
)

type Program

type Program struct {
	// contains filtered or unexported fields
}

func (*Program) BuildProgram

func (p *Program) BuildProgram(devices []*Device, options string) error

func (*Program) CreateKernel

func (p *Program) CreateKernel(name string) (*Kernel, error)

func (*Program) Release

func (p *Program) Release()

Jump to

Keyboard shortcuts

? : This menu
/ : Search site
f or F : Jump to
y or Y : Canonical URL