public static void Add()
{
CLResultCode error = CLResultCode.Success;
CLPlatform[] platforms = new CLPlatform[1];
CL.GetPlatformIds(1, platforms, out _);
CLDevice[] devices = new CLDevice[1];
CL.GetDeviceIds(platforms[0], DeviceType.All, 1, devices, out _);
CLContext context = CL.CreateContext(IntPtr.Zero, devices, IntPtr.Zero, IntPtr.Zero, out _);
CLProgram program =
CL.CreateProgramWithSource(context, File.ReadAllText("Kernels/add_arrays.cl"), out error);
error = CL.BuildProgram(program, 1, devices, null, IntPtr.Zero, IntPtr.Zero);
if (error != CLResultCode.Success)
{
throw new Exception(error.ToString());
}
CLKernel kernel = CL.CreateKernel(program, "add", out error);
Span <float> inputA = new float[]
{
1, 24, 5, 43, 41, 56
};
Span <float> inputB = new float[]
{
72, -323, -1, 43, -41, -26
};
Span <float> output = stackalloc float[inputA.Length];
CLBuffer bufferA = CL.CreateBuffer(context, MemoryFlags.ReadOnly | MemoryFlags.CopyHostPtr, inputA, out _);
CLBuffer bufferB = CL.CreateBuffer(context, MemoryFlags.ReadOnly | MemoryFlags.CopyHostPtr, inputB, out _);
CLBuffer outputBuffer = CL.CreateBuffer(context, MemoryFlags.WriteOnly, (UIntPtr)(output.Length * sizeof(float)), IntPtr.Zero, out _);
//For outputs I wouldn't use that also enqueueing a ReadBuffer is needed regardless
//CLBuffer outputBuffer = CL.CreateBuffer(context, MemoryFlags.WriteOnly | MemoryFlags.UseHostPtr, output, out _);
CL.SetKernelArg(kernel, 0, bufferA);
CL.SetKernelArg(kernel, 1, bufferB);
CL.SetKernelArg(kernel, 2, outputBuffer);
CLCommandQueue queue = CL.CreateCommandQueueWithProperties(context, devices[0], IntPtr.Zero, out error);
CL.EnqueueNDRangeKernel(queue, kernel, 1, null,
new[] { (UIntPtr)inputA.Length }, null, 0, null, out _);
CL.EnqueueReadBuffer(queue, outputBuffer, true, UIntPtr.Zero, output, null, out _);
foreach (float f in output)
{
Console.WriteLine(f);
}
CL.ReleaseMemoryObject(bufferA);
CL.ReleaseMemoryObject(bufferB);
CL.ReleaseMemoryObject(outputBuffer);
CL.ReleaseCommandQueue(queue);
CL.ReleaseKernel(kernel);
CL.ReleaseProgram(program);
CL.ReleaseContext(context);
}
static void Main(string[] args)
{
ToGrayscale.ConvertToGrayscale("image.jpg");
//Get the ids of available opencl platforms
CL.GetPlatformIds(0, null, out uint platformCount);
CLPlatform[] platformIds = new CLPlatform[platformCount];
CL.GetPlatformIds(platformCount, platformIds, out _);
Console.WriteLine(platformIds.Length);
foreach (CLPlatform platform in platformIds)
{
Console.WriteLine(platform.Handle);
CL.GetPlatformInfo(platform, PlatformInfo.Name, out byte[] val);
}
//Get the device ids for each platform
foreach (IntPtr platformId in platformIds)
{
CL.GetDeviceIds(new CLPlatform(platformId), DeviceType.All, out CLDevice[] deviceIds);
CLContext context = CL.CreateContext(IntPtr.Zero, (uint)deviceIds.Length, deviceIds, IntPtr.Zero,
IntPtr.Zero, out CLResultCode result);
if (result != CLResultCode.Success)
{
throw new Exception("The context couldn't be created.");
}
string code = @"
__kernel void add(__global float* A, __global float* B,__global float* result, const float mul)
{
int i = get_global_id(0);
result[i] = (A[i] + B[i])*mul;
}";
CLProgram program = CL.CreateProgramWithSource(context, code, out result);
CL.BuildProgram(program, (uint)deviceIds.Length, deviceIds, null, IntPtr.Zero, IntPtr.Zero);
CLKernel kernel = CL.CreateKernel(program, "add", out result);
int arraySize = 20;
float[] A = new float[arraySize];
float[] B = new float[arraySize];
for (int i = 0; i < arraySize; i++)
{
A[i] = 1;
B[i] = i;
}
CLBuffer bufferA = CL.CreateBuffer(context, MemoryFlags.ReadOnly | MemoryFlags.CopyHostPtr, A,
out result);
CLBuffer bufferB = CL.CreateBuffer(context, MemoryFlags.ReadOnly | MemoryFlags.CopyHostPtr, B,
out result);
float[] pattern = new float[] { 1, 3, 5, 7 };
CLBuffer resultBuffer = new CLBuffer(CL.CreateBuffer(context, MemoryFlags.WriteOnly,
new UIntPtr((uint)(arraySize * sizeof(float))), IntPtr.Zero, out result));
try
{
CL.SetKernelArg(kernel, 0, bufferA);
CL.SetKernelArg(kernel, 1, bufferB);
CL.SetKernelArg(kernel, 2, resultBuffer);
CL.SetKernelArg(kernel, 3, -1f);
CLCommandQueue commandQueue = new CLCommandQueue(
CL.CreateCommandQueueWithProperties(context, deviceIds[0], IntPtr.Zero, out result));
CL.EnqueueFillBuffer(commandQueue, bufferB, pattern, UIntPtr.Zero, (UIntPtr)(arraySize * sizeof(float)), null,
out _);
//CL.EnqueueNDRangeKernel(commandQueue, kernel, 1, null, new UIntPtr[] {new UIntPtr((uint)A.Length)},
// null, 0, null, out CLEvent eventHandle);
CL.EnqueueNDRangeKernel(commandQueue, kernel, 1, null, new UIntPtr[] { new UIntPtr((uint)A.Length) },
null, 0, null, out CLEvent eventHandle);
CL.Finish(commandQueue);
CL.SetEventCallback(eventHandle, (int)CommandExecutionStatus.Complete, (waitEvent, data) =>
{
float[] resultValues = new float[arraySize];
CL.EnqueueReadBuffer(commandQueue, resultBuffer, true, UIntPtr.Zero, resultValues, null, out _);
StringBuilder line = new StringBuilder();
foreach (float res in resultValues)
{
line.Append(res);
line.Append(", ");
}
Console.WriteLine(line.ToString());
});
//get rid of the buffers because we no longer need them
CL.ReleaseMemoryObject(bufferA);
CL.ReleaseMemoryObject(bufferB);
CL.ReleaseMemoryObject(resultBuffer);
//Release the program kernels and queues
CL.ReleaseProgram(program);
CL.ReleaseKernel(kernel);
CL.ReleaseCommandQueue(commandQueue);
CL.ReleaseContext(context);
CL.ReleaseEvent(eventHandle);
}
catch (Exception e)
{
Console.WriteLine(e.ToString());
throw;
}
}
}
public static void ConvertToGrayscale(string inputPath)
{
CLResultCode error = CLResultCode.Success;
//Get a platform
CLPlatform[] platforms = new CLPlatform[1];
CL.GetPlatformIds(1, platforms, out _);
//Get a device
CLDevice[] devices = new CLDevice[1];
CL.GetDeviceIds(platforms[0], DeviceType.Gpu, 1, devices, out _);
//Create a context
CLContext context = CL.CreateContext(IntPtr.Zero, devices, IntPtr.Zero, IntPtr.Zero, out error);
if (error != CLResultCode.Success)
{
throw new Exception("Error on creating a context");
}
//Create the program from source
CLProgram program =
CL.CreateProgramWithSource(context, File.ReadAllText("Kernels/grayscale.cl"), out error);
error = CL.BuildProgram(program, 1, devices, null, IntPtr.Zero, IntPtr.Zero);
if (error != CLResultCode.Success)
{
throw new Exception($"Error on building program: {error}");
}
//Get the kernel which we will use
CLKernel kernel = CL.CreateKernel(program, "grayscale", out error);
ImageFormat inputImageFormat = new ImageFormat
{
ChannelOrder = ChannelOrder.Bgra,
ChannelType = ChannelType.UnsignedInteger8
};
Bitmap inputBitmap = new Bitmap(inputPath);
BitmapData inputData = inputBitmap.LockBits(new Rectangle(0, 0, inputBitmap.Width, inputBitmap.Height),
ImageLockMode.ReadOnly, PixelFormat.Format32bppArgb);
ImageDescription imageDescription = new ImageDescription()
{
ImageType = MemoryObjectType.Image2D,
Width = (UIntPtr)inputBitmap.Width,
Height = (UIntPtr)inputBitmap.Height,
Depth = (UIntPtr)1
};
CLImage inputImage = CL.CreateImage(context, MemoryFlags.ReadOnly | MemoryFlags.CopyHostPtr,
ref inputImageFormat, ref imageDescription, inputData.Scan0, out error);
Bitmap outputBitmap = new Bitmap(inputBitmap.Width, inputBitmap.Height, PixelFormat.Format32bppArgb);
BitmapData outputData = outputBitmap.LockBits(new Rectangle(0, 0, inputBitmap.Width, inputBitmap.Height),
ImageLockMode.WriteOnly, PixelFormat.Format32bppArgb);
CLImage outputImage = CL.CreateImage(context, MemoryFlags.WriteOnly | MemoryFlags.UseHostPtr,
ref inputImageFormat, ref imageDescription, outputData.Scan0, out error);
CL.SetKernelArg(kernel, 0, rFact);
CL.SetKernelArg(kernel, 1, gFact);
CL.SetKernelArg(kernel, 2, bFact);
CL.SetKernelArg(kernel, 3, inputImage);
CL.SetKernelArg(kernel, 4, outputImage);
CLCommandQueue queue = CL.CreateCommandQueueWithProperties(context, devices[0], IntPtr.Zero, out error);
CL.EnqueueNDRangeKernel(queue, kernel, 2, new UIntPtr[] { UIntPtr.Zero, UIntPtr.Zero, }, new[]
{
(UIntPtr)inputBitmap.Width,
(UIntPtr)inputBitmap.Height,
}, null, 0, null, out _);
CL.EnqueueReadImage(queue, outputImage, 1, new UIntPtr[] { UIntPtr.Zero, UIntPtr.Zero, },
new UIntPtr[]
{
(UIntPtr)inputBitmap.Width,
(UIntPtr)inputBitmap.Height,
(UIntPtr)1,
}, UIntPtr.Zero, UIntPtr.Zero, outputData.Scan0, 0, null, out _);
outputBitmap.UnlockBits(outputData);
outputBitmap.Save("grayscale.png", System.Drawing.Imaging.ImageFormat.Png);
//Dispose of all things
inputBitmap.Dispose();
outputBitmap.Dispose();
CL.ReleaseMemoryObject(inputImage);
CL.ReleaseMemoryObject(outputImage);
CL.ReleaseCommandQueue(queue);
CL.ReleaseKernel(kernel);
CL.ReleaseProgram(program);
CL.ReleaseContext(context);
}
