我对整个 OpenCL 世界还是很陌生,我创建了两个非常简单的内核,我试图将它们链接在一起,但我得到了相当虚假的结果。当单独运行时,它们按预期工作,但是当它们一起运行时,那是我看到奇怪结果的时候。
所以,每个内核单独看起来像这样
矢量 3 噪声
__kernel void addVector3Noise( __global struct State* states, __global float3* randomVector3Values){
int stateNum = get_global_id(0);
struct State state = states[stateNum];
float3 randomVal = randomVector3Values[stateNum];
struct State newState;
newState.Vec3 = (float3)(state.Vec3.x + randomVal.x,state.Vec3.y + randomVal.y,state.Vec3.z + randomVal.z);
newState.Vec4 = state.Vec4;
states[stateNum] = newState;
}
为了测试这一点,所有状态都Vec3
具有[ 1.0f, 1.0f, 1.0f]
所有随机值都相同,所以我得到的输出是一个状态数组,其值[2.0f, 2.0f, 2.0f]
与我预期的一样。
矢量 4 噪声
__kernel void addVector4Noise(__global struct State* states,
__global float3* randomVector4Values){
int stateNum = get_global_id(0);
struct State state = states[stateNum];
float3 randomVal = randomVector4Values[stateNum];
float4 newVector4 = randomQuaternionRotation(state.Vector4, randomVal);
struct State newState;
newState.Vector3 = state.Vector3;
newState.Vector4= newVector4;
states[stateNum] = newState;
}
用非常简单的测试数据运行它也给了我想要的东西。
现在问题出现在将它们链接在一起时。我按照向量 4 噪声 -> 向量 3 噪声的顺序调用它们。现在,当运行 Vector 4 噪声内核时,我看到 vector 3 的值发生了变化,而且这种变化似乎遵循一种模式。
因此,在向量 4 内核运行之后,我希望每个状态中的向量 3 与插入时相同。这意味着每个状态的向量 3 值[1.0f,1.0f,1.0f]
如下实际上看到向量 3 的结果如下:
[1.0,1.0,1.0]
[0.576367259,1.0,1.0]
[0.999199867,0.6448302,1.0]
[1.313311, 1.067663, 0.3307195]
[-0.08005857, 1.067663, 1.450237]
[1, 0.2340522, 1.136126]
[1, 1, 0.3025152]
[1, 1, 1]
并且该模式在所有 Vector 3 值中重复出现。请注意,在内核中,它只是将 Vector3 从先前状态复制到新状态。
这就是我使用 OpenCL.Net 将它们链接在一起的方式
using (var env = "*".CreateCLEnvironment(DeviceType.Gpu))
{
var source = LoadProgram("kernels.cl");
var context = env.Context;
ErrorCode errorCode;
var program = Cl.CreateProgramWithSource(context, 1u, source, null, out errorCode);
CheckSuccess(errorCode);
errorCode = Cl.BuildProgram(program, (uint)env.Devices.Length, env.Devices, "-cl-opt-disable", null,
IntPtr.Zero);
if (errorCode != ErrorCode.Success)
{
var info = Cl.GetProgramBuildInfo(program, env.Devices[0], ProgramBuildInfo.Log, out errorCode).ToString();
throw new Exception(info);
}
var kernels = Cl.CreateKernelsInProgram(program, out errorCode);
CheckSuccess(errorCode);
var Vector4NoiseKernel = kernels[0];
var Vector3NoiseKernel = kernels[1];
var rnd = new Random();
var states = Enumerable.Range(1, ArrayLength)
.Select(_ => new State
{
Vector3 = new Vector3(1, 1, 1),
Vector4 = new Vector4(0.5f,0.5f,0.5f,0.5f)
})
.ToArray();
var randomVector4Values = Enumerable.Range(1, ArrayLength)
.Select(_ => new Vector3(2f, 2f, 2f))
.ToArray();
var randomVector3Values = Enumerable.Range(1, ArrayLength)
.Select(_ => new Vector3(1f, 1f, 1f))
.ToArray();
var vector4StatesBuffer = context.CreateBuffer(states, MemFlags.ReadWrite);
var randomVector4ValuesBuffer = context.CreateBuffer(randomVector4Values, MemFlags.ReadOnly);
Event ev;
Cl.SetKernelArg(vector4NoiseKernel, 0, vector4StatesBuffer);
Cl.SetKernelArg(vector4NoiseKernel, 1, randomVector4ValuesBuffer);
errorCode = Cl.EnqueueNDRangeKernel(env.CommandQueues[0], vector4NoiseKernel, 1, null
, new[] { new IntPtr(ArrayLength) }, new[] { new IntPtr(1) }, 0u, null, out ev);
errorCode.Check();
env.CommandQueues[0].ReadFromBuffer(vector4StatesBuffer, states, waitFor: ev);
var randomVector3ValuesBuffer = context.CreateBuffer(randomVector3Values, MemFlags.ReadOnly);
var vector3StatesBuffer = context.CreateBuffer(states, MemFlags.ReadWrite);
Cl.SetKernelArg(vector3NoiseKernel, 0, vector3StatesBuffer);
Cl.SetKernelArg(vector3NoiseKernel, 1, randomVector3ValuesBuffer);
errorCode = Cl.EnqueueNDRangeKernel(env.CommandQueues[0], vector3NoiseKernel, 1, null
, new[] { new IntPtr(ArrayLength) }, new[] { new IntPtr(1) }, 0u, null, out ev);
errorCode.Check();
Cl.Finish(env.CommandQueues[0]).Check();
env.CommandQueues[0].ReadFromBuffer(vector3StatesBuffer, states, waitFor: ev);
}
请原谅那里有大量代码,但这是一个游乐场项目,我几乎只是在吐槽想法,所以整洁和优雅在这里不是问题:)
提前感谢您提供的任何帮助。
编辑
所以我今天早上做的第一件事是将每个内核拉到自己的 cl 文件中,并确保每个内核都有自己的状态版本,只有它需要的状态(分别为 Vector4 和 Vector3),以及一个新的 using 语句与新分离出的 Vector3 噪声内核的所有 gubbins 一起使用。令我高兴的是,Vector4 噪声内核完全符合我的预期,但是,当涉及到 Vector3 噪声时,出现了与之前类似的问题。仍然[1.0f,1.0f,1.0f]
作为随机值和起始 Vector3 值传入,它仍然没有产生我期望的输出。这次重复的模式是:
[2.0f,2.0f,2.0f]
[1.0f,2.0f,2.0f]
[2.0f,1.0f,2.0f]
[2.0f,2.0f,1.0f]
[2.0f,2.0f,2.0f]