Lines Matching refs:clEnv
221 clEnv; in getOpenCLEnvironment() local
223 clEnv=GetCurrentOpenCLEnv(); in getOpenCLEnvironment()
224 if (clEnv == (MagickCLEnv) NULL) in getOpenCLEnvironment()
227 if (clEnv->enabled == MagickFalse) in getOpenCLEnvironment()
230 if (InitializeOpenCL(clEnv,exception) == MagickFalse) in getOpenCLEnvironment()
233 return(clEnv); in getOpenCLEnvironment()
312 static MagickBooleanType LaunchHistogramKernel(MagickCLEnv clEnv, in LaunchHistogramKernel() argument
355 clStatus=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in LaunchHistogramKernel()
356 clStatus|=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(ChannelType),&channel); in LaunchHistogramKernel()
357 clStatus|=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(cl_uint),&colorspace); in LaunchHistogramKernel()
358 clStatus|=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(cl_uint),&method); in LaunchHistogramKernel()
359 …clStatus|=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(cl_mem),(void *)&histogramBuff… in LaunchHistogramKernel()
370 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, histogramKernel, 2, NULL, global_work_siz… in LaunchHistogramKernel()
401 static Image *ComputeAddNoiseImage(const Image *image,MagickCLEnv clEnv, in ComputeAddNoiseImage() argument
457 device=RequestOpenCLDevice(clEnv); in ComputeAddNoiseImage()
611 static Image *ComputeBlurImage(const Image* image,MagickCLEnv clEnv, in ComputeBlurImage() argument
668 device=RequestOpenCLDevice(clEnv); in ComputeBlurImage()
796 clEnv; in AccelerateBlurImage() local
806 clEnv=getOpenCLEnvironment(exception); in AccelerateBlurImage()
807 if (clEnv == (MagickCLEnv) NULL) in AccelerateBlurImage()
810 filteredImage=ComputeBlurImage(image,clEnv,radius,sigma,exception); in AccelerateBlurImage()
826 static MagickBooleanType ComputeContrastImage(Image *image,MagickCLEnv clEnv, in ComputeContrastImage() argument
864 device=RequestOpenCLDevice(clEnv); in ComputeContrastImage()
919 clEnv; in AccelerateContrastImage() local
929 clEnv=getOpenCLEnvironment(exception); in AccelerateContrastImage()
930 if (clEnv == (MagickCLEnv) NULL) in AccelerateContrastImage()
933 status=ComputeContrastImage(image,clEnv,sharpen,exception); in AccelerateContrastImage()
950 MagickCLEnv clEnv,const double black_point,const double white_point, in ComputeContrastStretchImage() argument
1034 device = RequestOpenCLDevice(clEnv); in ComputeContrastStretchImage()
1083 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeContrastStretchImage()
1105 …histogramBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(cl_ui… in ComputeContrastStretchImage()
1112 …status = LaunchHistogramKernel(clEnv, device, queue, imageBuffer, histogramBuffer, image, image->c… in ComputeContrastStretchImage()
1120 …clEnv->library->clEnqueueMapBuffer(queue, histogramBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, l… in ComputeContrastStretchImage()
1125 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, histogramBuffer, CL_TRUE, 0, length * sizeof… in ComputeContrastStretchImage()
1136 …clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, histogramBuffer, histogram, 0, NULL, NUL… in ComputeContrastStretchImage()
1147 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeContrastStretchImage()
1366 …imageBuffer = clEnv->library->clCreateBuffer(context, mem_flags, length * sizeof(CLPixelPacket), (… in ComputeContrastStretchImage()
1387 …stretchMapBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(Pixe… in ComputeContrastStretchImage()
1404 clStatus=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeContrastStretchImage()
1405 …clStatus|=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(ChannelType),&image->channel_mas… in ComputeContrastStretchImage()
1406 …clStatus|=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(cl_mem),(void *)&stretchMapBuffe… in ComputeContrastStretchImage()
1407 clStatus|=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(cl_float4),&white); in ComputeContrastStretchImage()
1408 clStatus|=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(cl_float4),&black); in ComputeContrastStretchImage()
1419 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, stretchKernel, 2, NULL, global_work_size,… in ComputeContrastStretchImage()
1432 …clEnv->library->clEnqueueMapBuffer(queue, imageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, lengt… in ComputeContrastStretchImage()
1437 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, imageBuffer, CL_TRUE, 0, length * sizeof(CLP… in ComputeContrastStretchImage()
1452 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeContrastStretchImage()
1455 clEnv->library->clReleaseMemObject(stretchMapBuffer); in ComputeContrastStretchImage()
1459 clEnv->library->clReleaseMemObject(histogramBuffer); in ComputeContrastStretchImage()
1482 clEnv; in AccelerateContrastStretchImage() local
1493 clEnv=getOpenCLEnvironment(exception); in AccelerateContrastStretchImage()
1494 if (clEnv == (MagickCLEnv) NULL) in AccelerateContrastStretchImage()
1497 status=ComputeContrastStretchImage(image,clEnv,black_point,white_point, in AccelerateContrastStretchImage()
1514 static Image *ComputeConvolveImage(const Image* image,MagickCLEnv clEnv, in ComputeConvolveImage() argument
1590 device = RequestOpenCLDevice(clEnv); in ComputeConvolveImage()
1615 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeConvolveImage()
1649 …filteredImageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(C… in ComputeConvolveImage()
1657 …convolutionKernel = clEnv->library->clCreateBuffer(device->context, CL_MEM_READ_ONLY|CL_MEM_ALLOC_… in ComputeConvolveImage()
1666 …kernelBufferPtr = (float*)clEnv->library->clEnqueueMapBuffer(queue, convolutionKernel, CL_TRUE, CL… in ComputeConvolveImage()
1677 …clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, convolutionKernel, kernelBufferPtr, 0, N… in ComputeConvolveImage()
1710 clStatus =clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeConvolveImage()
1711 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&filteredImageBuffer); in ComputeConvolveImage()
1714 clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&imageWidth); in ComputeConvolveImage()
1715 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&imageHeight); in ComputeConvolveImage()
1716 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&convolutionKernel); in ComputeConvolveImage()
1719 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&filterWidth); in ComputeConvolveImage()
1720 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&filterHeight); in ComputeConvolveImage()
1722 clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&matte); in ComputeConvolveImage()
1723 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(ChannelType),(void *)&image->channel_… in ComputeConvolveImage()
1724 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++, (localGroupSize[0] + kernel->width-1)*(loca… in ComputeConvolveImage()
1725 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++, kernel->width*kernel->height*sizeof(float),… in ComputeConvolveImage()
1737 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, clkernel, 2, NULL, global_work_size, loca… in ComputeConvolveImage()
1757 clStatus =clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeConvolveImage()
1758 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&filteredImageBuffer); in ComputeConvolveImage()
1761 clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&imageWidth); in ComputeConvolveImage()
1762 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&imageHeight); in ComputeConvolveImage()
1763 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&convolutionKernel); in ComputeConvolveImage()
1766 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&filterWidth); in ComputeConvolveImage()
1767 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&filterHeight); in ComputeConvolveImage()
1769 clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&matte); in ComputeConvolveImage()
1770 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(ChannelType),(void *)&image->channel_… in ComputeConvolveImage()
1781 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, clkernel, 2, NULL, global_work_size, loca… in ComputeConvolveImage()
1794 …clEnv->library->clEnqueueMapBuffer(queue, filteredImageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, … in ComputeConvolveImage()
1799 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, filteredImageBuffer, CL_TRUE, 0, length * si… in ComputeConvolveImage()
1815 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeConvolveImage()
1817 clEnv->library->clReleaseMemObject(filteredImageBuffer); in ComputeConvolveImage()
1819 clEnv->library->clReleaseMemObject(convolutionKernel); in ComputeConvolveImage()
1874 static Image *ComputeDespeckleImage(const Image *image,MagickCLEnv clEnv, in ComputeDespeckleImage() argument
1948 device = RequestOpenCLDevice(clEnv); in ComputeDespeckleImage()
1969 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeDespeckleImage()
1980 …tempImageBuffer[k] = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CL… in ComputeDespeckleImage()
2015 …filteredImageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(C… in ComputeDespeckleImage()
2025 clStatus =clEnv->library->clSetKernelArg(hullPass1,0,sizeof(cl_mem),(void *)&imageBuffer); in ComputeDespeckleImage()
2026 clStatus |=clEnv->library->clSetKernelArg(hullPass1,1,sizeof(cl_mem),(void *)(tempImageBuffer+1)); in ComputeDespeckleImage()
2028 clStatus |=clEnv->library->clSetKernelArg(hullPass1,2,sizeof(unsigned int),(void *)&imageWidth); in ComputeDespeckleImage()
2030 clStatus |=clEnv->library->clSetKernelArg(hullPass1,3,sizeof(unsigned int),(void *)&imageHeight); in ComputeDespeckleImage()
2032 clStatus |=clEnv->library->clSetKernelArg(hullPass1,6,sizeof(int),(void *)&matte); in ComputeDespeckleImage()
2039 clStatus = clEnv->library->clSetKernelArg(hullPass2,0,sizeof(cl_mem),(void *)(tempImageBuffer+1)); in ComputeDespeckleImage()
2040 clStatus |=clEnv->library->clSetKernelArg(hullPass2,1,sizeof(cl_mem),(void *)tempImageBuffer); in ComputeDespeckleImage()
2042 clStatus |=clEnv->library->clSetKernelArg(hullPass2,2,sizeof(unsigned int),(void *)&imageWidth); in ComputeDespeckleImage()
2044 clStatus |=clEnv->library->clSetKernelArg(hullPass2,3,sizeof(unsigned int),(void *)&imageHeight); in ComputeDespeckleImage()
2046 clStatus |=clEnv->library->clSetKernelArg(hullPass2,6,sizeof(int),(void *)&matte); in ComputeDespeckleImage()
2067 clStatus = clEnv->library->clSetKernelArg(hullPass1,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2068 clStatus|= clEnv->library->clSetKernelArg(hullPass1,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2069 clStatus|=clEnv->library->clSetKernelArg(hullPass2,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2070 clStatus|=clEnv->library->clSetKernelArg(hullPass2,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2077 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass1, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2086 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass2, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2095 … clStatus =clEnv->library->clSetKernelArg(hullPass1,0,sizeof(cl_mem),(void *)(tempImageBuffer)); in ComputeDespeckleImage()
2099 clStatus = clEnv->library->clSetKernelArg(hullPass1,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2100 clStatus|= clEnv->library->clSetKernelArg(hullPass1,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2101 clStatus|=clEnv->library->clSetKernelArg(hullPass2,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2102 clStatus|=clEnv->library->clSetKernelArg(hullPass2,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2109 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass1, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2118 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass2, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2129 clStatus = clEnv->library->clSetKernelArg(hullPass1,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2130 clStatus|= clEnv->library->clSetKernelArg(hullPass1,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2131 clStatus|=clEnv->library->clSetKernelArg(hullPass2,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2132 clStatus|=clEnv->library->clSetKernelArg(hullPass2,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2139 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass1, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2148 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass2, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2159 clStatus = clEnv->library->clSetKernelArg(hullPass1,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2160 clStatus|= clEnv->library->clSetKernelArg(hullPass1,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2161 clStatus|=clEnv->library->clSetKernelArg(hullPass2,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2162 clStatus|=clEnv->library->clSetKernelArg(hullPass2,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2165 …clStatus |=clEnv->library->clSetKernelArg(hullPass2,1,sizeof(cl_mem),(void *)&filteredImageBuffer); in ComputeDespeckleImage()
2173 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass1, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2182 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass2, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2194 …clEnv->library->clEnqueueMapBuffer(queue, filteredImageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, … in ComputeDespeckleImage()
2199 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, filteredImageBuffer, CL_TRUE, 0, length * si… in ComputeDespeckleImage()
2220 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeDespeckleImage()
2224 clEnv->library->clReleaseMemObject(tempImageBuffer[k]); in ComputeDespeckleImage()
2227 clEnv->library->clReleaseMemObject(filteredImageBuffer); in ComputeDespeckleImage()
2245 clEnv; in AccelerateDespeckleImage() local
2253 clEnv=getOpenCLEnvironment(exception); in AccelerateDespeckleImage()
2254 if (clEnv == (MagickCLEnv) NULL) in AccelerateDespeckleImage()
2257 filteredImage=ComputeDespeckleImage(image,clEnv,exception); in AccelerateDespeckleImage()
2273 static MagickBooleanType ComputeEqualizeImage(Image *image,MagickCLEnv clEnv, in ComputeEqualizeImage() argument
2354 device = RequestOpenCLDevice(clEnv); in ComputeEqualizeImage()
2391 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeEqualizeImage()
2413 …histogramBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(cl_ui… in ComputeEqualizeImage()
2420 …status = LaunchHistogramKernel(clEnv, device, queue, imageBuffer, histogramBuffer, image, image->c… in ComputeEqualizeImage()
2428 …clEnv->library->clEnqueueMapBuffer(queue, histogramBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, l… in ComputeEqualizeImage()
2433 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, histogramBuffer, CL_TRUE, 0, length * sizeof… in ComputeEqualizeImage()
2444 …clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, histogramBuffer, histogram, 0, NULL, NUL… in ComputeEqualizeImage()
2455 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeEqualizeImage()
2575 …imageBuffer = clEnv->library->clCreateBuffer(context, mem_flags, length * sizeof(CLPixelPacket), (… in ComputeEqualizeImage()
2596 …equalizeMapBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(Pix… in ComputeEqualizeImage()
2613 clStatus=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeEqualizeImage()
2614 …clStatus|=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(ChannelType),&image->channel_ma… in ComputeEqualizeImage()
2615 …clStatus|=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(cl_mem),(void *)&equalizeMapBuf… in ComputeEqualizeImage()
2616 clStatus|=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(cl_float4),&white); in ComputeEqualizeImage()
2617 clStatus|=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(cl_float4),&black); in ComputeEqualizeImage()
2628 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, equalizeKernel, 2, NULL, global_work_size… in ComputeEqualizeImage()
2641 …clEnv->library->clEnqueueMapBuffer(queue, imageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, lengt… in ComputeEqualizeImage()
2646 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, imageBuffer, CL_TRUE, 0, length * sizeof(CLP… in ComputeEqualizeImage()
2661 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeEqualizeImage()
2665 clEnv->library->clReleaseMemObject(equalizeMapBuffer); in ComputeEqualizeImage()
2669 clEnv->library->clReleaseMemObject(histogramBuffer); in ComputeEqualizeImage()
2691 clEnv; in AccelerateEqualizeImage() local
2702 clEnv=getOpenCLEnvironment(exception); in AccelerateEqualizeImage()
2703 if (clEnv == (MagickCLEnv) NULL) in AccelerateEqualizeImage()
2706 status=ComputeEqualizeImage(image,clEnv,exception); in AccelerateEqualizeImage()
2722 static MagickBooleanType ComputeFunctionImage(Image *image,MagickCLEnv clEnv, in ComputeFunctionImage() argument
2766 device=RequestOpenCLDevice(clEnv); in ComputeFunctionImage()
2843 clEnv; in AccelerateFunctionImage() local
2853 clEnv=getOpenCLEnvironment(exception); in AccelerateFunctionImage()
2854 if (clEnv == (MagickCLEnv) NULL) in AccelerateFunctionImage()
2857 status=ComputeFunctionImage(image,clEnv,function,number_parameters, in AccelerateFunctionImage()
2874 static MagickBooleanType ComputeGrayscaleImage(Image *image,MagickCLEnv clEnv, in ComputeGrayscaleImage() argument
2913 device=RequestOpenCLDevice(clEnv); in ComputeGrayscaleImage()
2970 clEnv; in AccelerateGrayscaleImage() local
2989 clEnv=getOpenCLEnvironment(exception); in AccelerateGrayscaleImage()
2990 if (clEnv == (MagickCLEnv) NULL) in AccelerateGrayscaleImage()
2993 status=ComputeGrayscaleImage(image,clEnv,method,exception); in AccelerateGrayscaleImage()
3009 static Image *ComputeLocalContrastImage(const Image *image,MagickCLEnv clEnv, in ComputeLocalContrastImage() argument
3075 device = RequestOpenCLDevice(clEnv); in ComputeLocalContrastImage()
3101 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeLocalContrastImage()
3139 …filteredImageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(C… in ComputeLocalContrastImage()
3151 …tempImageBuffer = clEnv->library->clCreateBuffer(device->context, CL_MEM_READ_WRITE, length * size… in ComputeLocalContrastImage()
3186 … clStatus=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeLocalContrastImage()
3187 …clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(cl_mem),(void *)&filteredImageBu… in ComputeLocalContrastImage()
3188 …clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(cl_mem),(void *)&tempImageBuffer… in ComputeLocalContrastImage()
3189 clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(cl_int),(void *)&iRadius); in ComputeLocalContrastImage()
3190 …clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(unsigned int),(void *)&imageColu… in ComputeLocalContrastImage()
3191 …clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(unsigned int),(void *)&imageRows… in ComputeLocalContrastImage()
3215 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, blurRowKernel, 2, goffset, gsize, wsize, … in ComputeLocalContrastImage()
3221 clEnv->library->clFlush(queue); in ComputeLocalContrastImage()
3229 … clStatus=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeLocalContrastImage()
3230 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(cl_mem),(void *)&filteredImag… in ComputeLocalContrastImage()
3231 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(cl_mem),(void *)&tempImageBuf… in ComputeLocalContrastImage()
3232 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(unsigned int),(void *)&iRadiu… in ComputeLocalContrastImage()
3233 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(cl_float),(void *)&FStrength); in ComputeLocalContrastImage()
3234 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(unsigned int),(void *)&imageC… in ComputeLocalContrastImage()
3235 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(unsigned int),(void *)&imageR… in ComputeLocalContrastImage()
3259 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, blurColumnKernel, 2, goffset, gsize, wsiz… in ComputeLocalContrastImage()
3265 clEnv->library->clFlush(queue); in ComputeLocalContrastImage()
3275 …clEnv->library->clEnqueueMapBuffer(queue, filteredImageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, … in ComputeLocalContrastImage()
3280 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, filteredImageBuffer, CL_TRUE, 0, length * si… in ComputeLocalContrastImage()
3297 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeLocalContrastImage()
3299 clEnv->library->clReleaseMemObject(filteredImageBuffer); in ComputeLocalContrastImage()
3301 clEnv->library->clReleaseMemObject(tempImageBuffer); in ComputeLocalContrastImage()
3303 clEnv->library->clReleaseMemObject(imageKernelBuffer); in ComputeLocalContrastImage()
3331 clEnv; in AccelerateLocalContrastImage() local
3339 clEnv=getOpenCLEnvironment(exception); in AccelerateLocalContrastImage()
3340 if (clEnv == (MagickCLEnv) NULL) in AccelerateLocalContrastImage()
3343 filteredImage=ComputeLocalContrastImage(image,clEnv,radius,strength, in AccelerateLocalContrastImage()
3360 static MagickBooleanType ComputeModulateImage(Image *image,MagickCLEnv clEnv, in ComputeModulateImage() argument
3419 device = RequestOpenCLDevice(clEnv); in ComputeModulateImage()
3450 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeModulateImage()
3470 clStatus=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeModulateImage()
3471 clStatus|=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_float),&bright); in ComputeModulateImage()
3472 clStatus|=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_float),&hue); in ComputeModulateImage()
3473 clStatus|=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_float),&saturation); in ComputeModulateImage()
3474 clStatus|=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_float),&color); in ComputeModulateImage()
3486 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, modulateKernel, 2, NULL, global_work_size… in ComputeModulateImage()
3498 …clEnv->library->clEnqueueMapBuffer(queue, imageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, lengt… in ComputeModulateImage()
3503 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, imageBuffer, CL_TRUE, 0, length * sizeof(CLP… in ComputeModulateImage()
3518 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeModulateImage()
3539 clEnv; in AccelerateModulateImage() local
3552 clEnv=getOpenCLEnvironment(exception); in AccelerateModulateImage()
3553 if (clEnv == (MagickCLEnv) NULL) in AccelerateModulateImage()
3556 status=ComputeModulateImage(image,clEnv,percent_brightness,percent_hue, in AccelerateModulateImage()
3573 static Image* ComputeMotionBlurImage(const Image *image,MagickCLEnv clEnv, in ComputeMotionBlurImage() argument
3657 device = RequestOpenCLDevice(clEnv); in ComputeMotionBlurImage()
3688 imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, in ComputeMotionBlurImage()
3730 filteredImageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, in ComputeMotionBlurImage()
3740 imageKernelBuffer = clEnv->library->clCreateBuffer(device->context, in ComputeMotionBlurImage()
3751 kernelBufferPtr = (float*)clEnv->library->clEnqueueMapBuffer(queue, imageKernelBuffer, in ComputeMotionBlurImage()
3763 clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, imageKernelBuffer, kernelBufferPtr, in ComputeMotionBlurImage()
3772 offsetBuffer = clEnv->library->clCreateBuffer(device->context, in ComputeMotionBlurImage()
3782 offsetBufferPtr = (int*)clEnv->library->clEnqueueMapBuffer(queue, offsetBuffer, CL_TRUE, in ComputeMotionBlurImage()
3795 clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, offsetBuffer, offsetBufferPtr, 0, in ComputeMotionBlurImage()
3820 clStatus=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_mem), in ComputeMotionBlurImage()
3822 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_mem), in ComputeMotionBlurImage()
3826 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(unsigned int), in ComputeMotionBlurImage()
3828 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(unsigned int), in ComputeMotionBlurImage()
3830 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_mem), in ComputeMotionBlurImage()
3832 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(unsigned int), in ComputeMotionBlurImage()
3834 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_mem), in ComputeMotionBlurImage()
3842 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_float4), &biasPixel); in ComputeMotionBlurImage()
3844 …clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(ChannelType), &image->channel… in ComputeMotionBlurImage()
3846 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(unsigned int), &matte); in ComputeMotionBlurImage()
3863 clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, motionBlurKernel, 2, NULL, in ComputeMotionBlurImage()
3877 clEnv->library->clEnqueueMapBuffer(queue, filteredImageBuffer, CL_TRUE, in ComputeMotionBlurImage()
3884 clStatus = clEnv->library->clEnqueueReadBuffer(queue, filteredImageBuffer, CL_TRUE, 0, in ComputeMotionBlurImage()
3902 clEnv->library->clReleaseMemObject(filteredImageBuffer); in ComputeMotionBlurImage()
3904 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeMotionBlurImage()
3906 clEnv->library->clReleaseMemObject(imageKernelBuffer); in ComputeMotionBlurImage()
3927 clEnv; in AccelerateMotionBlurImage() local
3937 clEnv=getOpenCLEnvironment(exception); in AccelerateMotionBlurImage()
3938 if (clEnv == (MagickCLEnv) NULL) in AccelerateMotionBlurImage()
3941 filteredImage=ComputeMotionBlurImage(image,clEnv,kernel,width,offset, in AccelerateMotionBlurImage()
4325 static Image *ComputeResizeImage(const Image* image,MagickCLEnv clEnv, in ComputeResizeImage() argument
4371 device=RequestOpenCLDevice(clEnv); in ComputeResizeImage()
4502 clEnv; in AccelerateResizeImage() local
4516 clEnv=getOpenCLEnvironment(exception); in AccelerateResizeImage()
4517 if (clEnv == (MagickCLEnv) NULL) in AccelerateResizeImage()
4520 filteredImage=ComputeResizeImage(image,clEnv,resizedColumns,resizedRows, in AccelerateResizeImage()
4537 static Image* ComputeRotationalBlurImage(const Image *image,MagickCLEnv clEnv, in ComputeRotationalBlurImage() argument
4595 device=RequestOpenCLDevice(clEnv); in ComputeRotationalBlurImage()
4707 clEnv; in AccelerateRotationalBlurImage() local
4717 clEnv=getOpenCLEnvironment(exception); in AccelerateRotationalBlurImage()
4718 if (clEnv == (MagickCLEnv) NULL) in AccelerateRotationalBlurImage()
4721 filteredImage=ComputeRotationalBlurImage(image,clEnv,angle,exception); in AccelerateRotationalBlurImage()
4737 static Image *ComputeUnsharpMaskImage(const Image *image,MagickCLEnv clEnv, in ComputeUnsharpMaskImage() argument
4796 device=RequestOpenCLDevice(clEnv); in ComputeUnsharpMaskImage()
4929 MagickCLEnv clEnv,const double radius,const double sigma,const double gain, in ComputeUnsharpMaskImageSingle() argument
4977 device=RequestOpenCLDevice(clEnv); in ComputeUnsharpMaskImageSingle()
5062 clEnv; in AccelerateUnsharpMaskImage() local
5070 clEnv=getOpenCLEnvironment(exception); in AccelerateUnsharpMaskImage()
5071 if (clEnv == (MagickCLEnv) NULL) in AccelerateUnsharpMaskImage()
5075 filteredImage=ComputeUnsharpMaskImageSingle(image,clEnv,radius,sigma,gain, in AccelerateUnsharpMaskImage()
5078 filteredImage=ComputeUnsharpMaskImage(image,clEnv,radius,sigma,gain, in AccelerateUnsharpMaskImage()
5083 static Image *ComputeWaveletDenoiseImage(const Image *image,MagickCLEnv clEnv, in ComputeWaveletDenoiseImage() argument
5140 device=RequestOpenCLDevice(clEnv); in ComputeWaveletDenoiseImage()
5232 clEnv; in AccelerateWaveletDenoiseImage() local
5240 clEnv=getOpenCLEnvironment(exception); in AccelerateWaveletDenoiseImage()
5241 if (clEnv == (MagickCLEnv) NULL) in AccelerateWaveletDenoiseImage()
5244 filteredImage=ComputeWaveletDenoiseImage(image,clEnv,threshold,exception); in AccelerateWaveletDenoiseImage()