oclContext::oclContext(cl_context iContext, cl_platform_id iPlatform, char* iVendor)
: oclObject("")
, mContext(iContext)
, mVendor(VENDOR_UNKNOWN)
, mPlatform(iPlatform)
{
if (!strcmp(iVendor, VENDOR_NVIDIA))
{
mVendor = VENDOR_NVIDIA;
}
else if (!strcmp(iVendor, VENDOR_AMD))
{
mVendor = VENDOR_AMD;
}
else if (!strncmp(iVendor, VENDOR_INTEL, 5))
{
mVendor = VENDOR_INTEL;
}
setName(mVendor);
size_t lDeviceCount;
sStatusCL = clGetContextInfo(mContext, CL_CONTEXT_DEVICES, 0, NULL, &lDeviceCount);
oclSuccess("clGetContextInfo", this);
cl_device_id* lDevice = new cl_device_id[lDeviceCount];
clGetContextInfo(mContext, CL_CONTEXT_DEVICES, lDeviceCount, lDevice, NULL);
for (cl_uint i=0; i<lDeviceCount/sizeof(cl_device_id); i++)
{
mDevices.push_back(new oclDevice(*this, lDevice[i]));
}
delete [] lDevice;
};
bool operator() (oclProgram& iSource)
{
// call all the fluid kernels except clipBox
size_t lPartcleCount = mFluid.getParticleCount();
sStatusCL = clEnqueueNDRangeKernel(mDevice, *clIntegrateForce, 1, NULL, &lPartcleCount, &mFluid.cLocalSize, 0, NULL, clIntegrateForce->getEvent());
if (!oclSuccess("clEnqueueNDRangeKernel", &mFluid))
{
return false;
}
sStatusCL = clEnqueueNDRangeKernel(mDevice, *clGravity, 1, NULL, &lPartcleCount, &mFluid.cLocalSize, 0, NULL, clGravity->getEvent());
if (!oclSuccess("clEnqueueNDRangeKernel", &mFluid))
{
return false;
}
sStatusCL = clEnqueueNDRangeKernel(mDevice, *clIntegrateVelocity, 1, NULL, &lPartcleCount, &mFluid.cLocalSize, 0, NULL, clIntegrateVelocity->getEvent());
if (!oclSuccess("clEnqueueNDRangeKernel", &mFluid))
{
return false;
}
return 1;
}
oclContext* oclContext::create(const char* iVendor, int iDeviceType)
{
/*
cl_int status = CL_SUCCESS;
cl_device_type dType = CL_DEVICE_TYPE_GPU;
cl_uint numPlatforms;
cl_platform_id platform = NULL;
status = clGetPlatformIDs(0, NULL, &numPlatforms);
if (0 < numPlatforms)
{
cl_platform_id* platforms = new cl_platform_id[numPlatforms];
status = clGetPlatformIDs(numPlatforms, platforms, NULL);
for (unsigned i = 0; i < numPlatforms; ++i)
{
char pbuf[100];
status = clGetPlatformInfo(platforms[i],
CL_PLATFORM_VENDOR,
sizeof(pbuf),
pbuf,
NULL);
platform = platforms[i];
if (!strcmp(pbuf, "Advanced Micro Devices, Inc."))
{
break;
}
}
delete[] platforms;
}
#ifdef _WIN32
HGLRC glCtx = wglGetCurrentContext();
#else //!_WIN32
GLXContext glCtx = glXGetCurrentContext();
#endif //!_WIN32
cl_context_properties cpsGL[] = { CL_CONTEXT_PLATFORM, (cl_context_properties)platform,
#ifdef _WIN32
CL_WGL_HDC_KHR, (intptr_t) wglGetCurrentDC(),
#else //!_WIN32
CL_GLX_DISPLAY_KHR, (intptr_t) glXGetCurrentDisplay(),
#endif //!_WIN32
CL_GL_CONTEXT_KHR, (intptr_t) glCtx, 0};
cl_context context = clCreateContextFromType(
cpsGL,
dType,
NULL,
NULL,
&status);
return new oclContext(context, "Advanced Micro Devices, Inc.");
*/
cl_uint lPlatformCount = 0;
sStatusCL = clGetPlatformIDs(0, NULL, &lPlatformCount);
oclSuccess("clGetPlatformIDs");
clGetGLContextInfoKHR_fn _clGetGLContextInfoKHR = (clGetGLContextInfoKHR_fn)clGetExtensionFunctionAddress("clGetGLContextInfoKHR");
cl_platform_id lPlatform[100];
sStatusCL = clGetPlatformIDs(lPlatformCount, lPlatform, NULL);
oclSuccess("clGetPlatformIDs");
char lBuffer[200];
for (cl_uint i=0; i < lPlatformCount; i++)
{
sStatusCL = clGetPlatformInfo(lPlatform[i],
CL_PLATFORM_VENDOR,
sizeof(lBuffer),
lBuffer,
NULL);
oclSuccess("clGetPlatformInfo");
cl_context_properties GL_PROPS[] =
{
#ifdef WIN32
CL_GL_CONTEXT_KHR, (cl_context_properties)wglGetCurrentContext(),
CL_WGL_HDC_KHR, (cl_context_properties)wglGetCurrentDC(),
#else
CL_GL_CONTEXT_KHR, (cl_context_properties)glXGetCurrentContext(),
CL_GLX_DISPLAY_KHR, (intptr_t) glXGetCurrentDisplay(),
#endif
CL_CONTEXT_PLATFORM, (cl_context_properties)lPlatform[i],
0
};
cl_context_properties CL_PROPS[] =
{
CL_CONTEXT_PLATFORM, (cl_context_properties)lPlatform[i],
0
};
if (!strncmp(lBuffer, iVendor, 5)) // compare only first 5 letters -- Intel starts with "Intel" and "Intel(R)"
{
switch (iDeviceType)
{
case CL_DEVICE_TYPE_GPU:
// gpu context
cl_device_id lDevices[100];
cl_uint lDeviceCount;
sStatusCL = clGetDeviceIDs(lPlatform[i], CL_DEVICE_TYPE_GPU, 100, lDevices, &lDeviceCount);
if (!oclSuccess("clGetDeviceIDs"))
{
continue;
}
if (lDeviceCount)
{
size_t lDeviceGLCount = 0;
cl_device_id lDeviceGL;
sStatusCL = _clGetGLContextInfoKHR(GL_PROPS, CL_CURRENT_DEVICE_FOR_GL_CONTEXT_KHR, sizeof(cl_device_id), &lDeviceGL, &lDeviceGLCount);
if (!oclSuccess("clGetDeviceIDs"))
{
//continue; AMD drivers produce an error here if not OpenGL context is present
}
if (lDeviceGLCount)
{
// gpu context with sharing enabled
cl_context lContextCL = clCreateContext(GL_PROPS, lDeviceCount, lDevices, NULL, NULL, &sStatusCL);
if (!oclSuccess("clCreateContext"))
{
continue;
}
return new oclContext(lContextCL, lPlatform[i], lBuffer);
}
else
{
// gpu context without sharing
cl_context lContextCL = clCreateContext(CL_PROPS, lDeviceCount, lDevices, NULL, NULL, &sStatusCL);
if (!oclSuccess("clCreateContext"))
{
continue;
}
return new oclContext(lContextCL, lPlatform[i], lBuffer);
}
}
break;
case CL_DEVICE_TYPE_CPU:
// cpu context
cl_context lContextCL = clCreateContextFromType(CL_PROPS, CL_DEVICE_TYPE_CPU, NULL, NULL, &sStatusCL);
if (!oclSuccess("clCreateContextFromType"))
{
continue;
}
return new oclContext(lContextCL, lPlatform[i], lBuffer);
break;
}
}
}
return 0;
}
