Lines Matching refs:clEnv
220 clEnv; in getOpenCLEnvironment() local
222 clEnv=GetCurrentOpenCLEnv(); in getOpenCLEnvironment()
223 if (clEnv == (MagickCLEnv) NULL) in getOpenCLEnvironment()
226 if (clEnv->enabled == MagickFalse) in getOpenCLEnvironment()
229 if (InitializeOpenCL(clEnv,exception) == MagickFalse) in getOpenCLEnvironment()
232 return(clEnv); in getOpenCLEnvironment()
311 static MagickBooleanType LaunchHistogramKernel(MagickCLEnv clEnv, in LaunchHistogramKernel() argument
354 clStatus=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in LaunchHistogramKernel()
355 clStatus|=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(ChannelType),&channel); in LaunchHistogramKernel()
356 clStatus|=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(cl_uint),&colorspace); in LaunchHistogramKernel()
357 clStatus|=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(cl_uint),&method); in LaunchHistogramKernel()
358 …clStatus|=clEnv->library->clSetKernelArg(histogramKernel,i++,sizeof(cl_mem),(void *)&histogramBuff… in LaunchHistogramKernel()
369 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, histogramKernel, 2, NULL, global_work_siz… in LaunchHistogramKernel()
400 static Image *ComputeAddNoiseImage(const Image *image,MagickCLEnv clEnv, in ComputeAddNoiseImage() argument
456 device=RequestOpenCLDevice(clEnv); in ComputeAddNoiseImage()
610 static Image *ComputeBlurImage(const Image* image,MagickCLEnv clEnv, in ComputeBlurImage() argument
667 device=RequestOpenCLDevice(clEnv); in ComputeBlurImage()
795 clEnv; in AccelerateBlurImage() local
805 clEnv=getOpenCLEnvironment(exception); in AccelerateBlurImage()
806 if (clEnv == (MagickCLEnv) NULL) in AccelerateBlurImage()
809 filteredImage=ComputeBlurImage(image,clEnv,radius,sigma,exception); in AccelerateBlurImage()
825 static MagickBooleanType ComputeContrastImage(Image *image,MagickCLEnv clEnv, in ComputeContrastImage() argument
863 device=RequestOpenCLDevice(clEnv); in ComputeContrastImage()
918 clEnv; in AccelerateContrastImage() local
928 clEnv=getOpenCLEnvironment(exception); in AccelerateContrastImage()
929 if (clEnv == (MagickCLEnv) NULL) in AccelerateContrastImage()
932 status=ComputeContrastImage(image,clEnv,sharpen,exception); in AccelerateContrastImage()
949 MagickCLEnv clEnv,const double black_point,const double white_point, in ComputeContrastStretchImage() argument
1033 device = RequestOpenCLDevice(clEnv); in ComputeContrastStretchImage()
1082 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeContrastStretchImage()
1104 …histogramBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(cl_ui… in ComputeContrastStretchImage()
1111 …status = LaunchHistogramKernel(clEnv, device, queue, imageBuffer, histogramBuffer, image, image->c… in ComputeContrastStretchImage()
1119 …clEnv->library->clEnqueueMapBuffer(queue, histogramBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, l… in ComputeContrastStretchImage()
1124 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, histogramBuffer, CL_TRUE, 0, length * sizeof… in ComputeContrastStretchImage()
1135 …clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, histogramBuffer, histogram, 0, NULL, NUL… in ComputeContrastStretchImage()
1146 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeContrastStretchImage()
1365 …imageBuffer = clEnv->library->clCreateBuffer(context, mem_flags, length * sizeof(CLPixelPacket), (… in ComputeContrastStretchImage()
1386 …stretchMapBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(Pixe… in ComputeContrastStretchImage()
1403 clStatus=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeContrastStretchImage()
1404 …clStatus|=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(ChannelType),&image->channel_mas… in ComputeContrastStretchImage()
1405 …clStatus|=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(cl_mem),(void *)&stretchMapBuffe… in ComputeContrastStretchImage()
1406 clStatus|=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(cl_float4),&white); in ComputeContrastStretchImage()
1407 clStatus|=clEnv->library->clSetKernelArg(stretchKernel,i++,sizeof(cl_float4),&black); in ComputeContrastStretchImage()
1418 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, stretchKernel, 2, NULL, global_work_size,… in ComputeContrastStretchImage()
1431 …clEnv->library->clEnqueueMapBuffer(queue, imageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, lengt… in ComputeContrastStretchImage()
1436 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, imageBuffer, CL_TRUE, 0, length * sizeof(CLP… in ComputeContrastStretchImage()
1451 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeContrastStretchImage()
1454 clEnv->library->clReleaseMemObject(stretchMapBuffer); in ComputeContrastStretchImage()
1458 clEnv->library->clReleaseMemObject(histogramBuffer); in ComputeContrastStretchImage()
1481 clEnv; in AccelerateContrastStretchImage() local
1492 clEnv=getOpenCLEnvironment(exception); in AccelerateContrastStretchImage()
1493 if (clEnv == (MagickCLEnv) NULL) in AccelerateContrastStretchImage()
1496 status=ComputeContrastStretchImage(image,clEnv,black_point,white_point, in AccelerateContrastStretchImage()
1513 static Image *ComputeConvolveImage(const Image* image,MagickCLEnv clEnv, in ComputeConvolveImage() argument
1589 device = RequestOpenCLDevice(clEnv); in ComputeConvolveImage()
1614 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeConvolveImage()
1648 …filteredImageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(C… in ComputeConvolveImage()
1656 …convolutionKernel = clEnv->library->clCreateBuffer(device->context, CL_MEM_READ_ONLY|CL_MEM_ALLOC_… in ComputeConvolveImage()
1665 …kernelBufferPtr = (float*)clEnv->library->clEnqueueMapBuffer(queue, convolutionKernel, CL_TRUE, CL… in ComputeConvolveImage()
1676 …clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, convolutionKernel, kernelBufferPtr, 0, N… in ComputeConvolveImage()
1709 clStatus =clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeConvolveImage()
1710 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&filteredImageBuffer); in ComputeConvolveImage()
1713 clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&imageWidth); in ComputeConvolveImage()
1714 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&imageHeight); in ComputeConvolveImage()
1715 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&convolutionKernel); in ComputeConvolveImage()
1718 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&filterWidth); in ComputeConvolveImage()
1719 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&filterHeight); in ComputeConvolveImage()
1721 clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&matte); in ComputeConvolveImage()
1722 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(ChannelType),(void *)&image->channel_… in ComputeConvolveImage()
1723 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++, (localGroupSize[0] + kernel->width-1)*(loca… in ComputeConvolveImage()
1724 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++, kernel->width*kernel->height*sizeof(float),… in ComputeConvolveImage()
1736 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, clkernel, 2, NULL, global_work_size, loca… in ComputeConvolveImage()
1756 clStatus =clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeConvolveImage()
1757 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&filteredImageBuffer); in ComputeConvolveImage()
1760 clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&imageWidth); in ComputeConvolveImage()
1761 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&imageHeight); in ComputeConvolveImage()
1762 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(cl_mem),(void *)&convolutionKernel); in ComputeConvolveImage()
1765 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&filterWidth); in ComputeConvolveImage()
1766 … clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&filterHeight); in ComputeConvolveImage()
1768 clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(unsigned int),(void *)&matte); in ComputeConvolveImage()
1769 …clStatus|=clEnv->library->clSetKernelArg(clkernel,i++,sizeof(ChannelType),(void *)&image->channel_… in ComputeConvolveImage()
1780 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, clkernel, 2, NULL, global_work_size, loca… in ComputeConvolveImage()
1793 …clEnv->library->clEnqueueMapBuffer(queue, filteredImageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, … in ComputeConvolveImage()
1798 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, filteredImageBuffer, CL_TRUE, 0, length * si… in ComputeConvolveImage()
1814 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeConvolveImage()
1816 clEnv->library->clReleaseMemObject(filteredImageBuffer); in ComputeConvolveImage()
1818 clEnv->library->clReleaseMemObject(convolutionKernel); in ComputeConvolveImage()
1873 static Image *ComputeDespeckleImage(const Image *image,MagickCLEnv clEnv, in ComputeDespeckleImage() argument
1947 device = RequestOpenCLDevice(clEnv); in ComputeDespeckleImage()
1968 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeDespeckleImage()
1979 …tempImageBuffer[k] = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CL… in ComputeDespeckleImage()
2014 …filteredImageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(C… in ComputeDespeckleImage()
2024 clStatus =clEnv->library->clSetKernelArg(hullPass1,0,sizeof(cl_mem),(void *)&imageBuffer); in ComputeDespeckleImage()
2025 clStatus |=clEnv->library->clSetKernelArg(hullPass1,1,sizeof(cl_mem),(void *)(tempImageBuffer+1)); in ComputeDespeckleImage()
2027 clStatus |=clEnv->library->clSetKernelArg(hullPass1,2,sizeof(unsigned int),(void *)&imageWidth); in ComputeDespeckleImage()
2029 clStatus |=clEnv->library->clSetKernelArg(hullPass1,3,sizeof(unsigned int),(void *)&imageHeight); in ComputeDespeckleImage()
2031 clStatus |=clEnv->library->clSetKernelArg(hullPass1,6,sizeof(int),(void *)&matte); in ComputeDespeckleImage()
2038 clStatus = clEnv->library->clSetKernelArg(hullPass2,0,sizeof(cl_mem),(void *)(tempImageBuffer+1)); in ComputeDespeckleImage()
2039 clStatus |=clEnv->library->clSetKernelArg(hullPass2,1,sizeof(cl_mem),(void *)tempImageBuffer); in ComputeDespeckleImage()
2041 clStatus |=clEnv->library->clSetKernelArg(hullPass2,2,sizeof(unsigned int),(void *)&imageWidth); in ComputeDespeckleImage()
2043 clStatus |=clEnv->library->clSetKernelArg(hullPass2,3,sizeof(unsigned int),(void *)&imageHeight); in ComputeDespeckleImage()
2045 clStatus |=clEnv->library->clSetKernelArg(hullPass2,6,sizeof(int),(void *)&matte); in ComputeDespeckleImage()
2066 clStatus = clEnv->library->clSetKernelArg(hullPass1,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2067 clStatus|= clEnv->library->clSetKernelArg(hullPass1,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2068 clStatus|=clEnv->library->clSetKernelArg(hullPass2,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2069 clStatus|=clEnv->library->clSetKernelArg(hullPass2,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2076 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass1, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2085 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass2, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2094 … clStatus =clEnv->library->clSetKernelArg(hullPass1,0,sizeof(cl_mem),(void *)(tempImageBuffer)); in ComputeDespeckleImage()
2098 clStatus = clEnv->library->clSetKernelArg(hullPass1,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2099 clStatus|= clEnv->library->clSetKernelArg(hullPass1,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2100 clStatus|=clEnv->library->clSetKernelArg(hullPass2,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2101 clStatus|=clEnv->library->clSetKernelArg(hullPass2,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2108 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass1, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2117 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass2, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2128 clStatus = clEnv->library->clSetKernelArg(hullPass1,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2129 clStatus|= clEnv->library->clSetKernelArg(hullPass1,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2130 clStatus|=clEnv->library->clSetKernelArg(hullPass2,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2131 clStatus|=clEnv->library->clSetKernelArg(hullPass2,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2138 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass1, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2147 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass2, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2158 clStatus = clEnv->library->clSetKernelArg(hullPass1,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2159 clStatus|= clEnv->library->clSetKernelArg(hullPass1,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2160 clStatus|=clEnv->library->clSetKernelArg(hullPass2,4,sizeof(cl_int2),(void *)&offset); in ComputeDespeckleImage()
2161 clStatus|=clEnv->library->clSetKernelArg(hullPass2,5,sizeof(int),(void *)&polarity); in ComputeDespeckleImage()
2164 …clStatus |=clEnv->library->clSetKernelArg(hullPass2,1,sizeof(cl_mem),(void *)&filteredImageBuffer); in ComputeDespeckleImage()
2172 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass1, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2181 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, hullPass2, 2, NULL, global_work_size, NUL… in ComputeDespeckleImage()
2193 …clEnv->library->clEnqueueMapBuffer(queue, filteredImageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, … in ComputeDespeckleImage()
2198 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, filteredImageBuffer, CL_TRUE, 0, length * si… in ComputeDespeckleImage()
2219 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeDespeckleImage()
2223 clEnv->library->clReleaseMemObject(tempImageBuffer[k]); in ComputeDespeckleImage()
2226 clEnv->library->clReleaseMemObject(filteredImageBuffer); in ComputeDespeckleImage()
2244 clEnv; in AccelerateDespeckleImage() local
2252 clEnv=getOpenCLEnvironment(exception); in AccelerateDespeckleImage()
2253 if (clEnv == (MagickCLEnv) NULL) in AccelerateDespeckleImage()
2256 filteredImage=ComputeDespeckleImage(image,clEnv,exception); in AccelerateDespeckleImage()
2272 static MagickBooleanType ComputeEqualizeImage(Image *image,MagickCLEnv clEnv, in ComputeEqualizeImage() argument
2353 device = RequestOpenCLDevice(clEnv); in ComputeEqualizeImage()
2390 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeEqualizeImage()
2412 …histogramBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(cl_ui… in ComputeEqualizeImage()
2419 …status = LaunchHistogramKernel(clEnv, device, queue, imageBuffer, histogramBuffer, image, image->c… in ComputeEqualizeImage()
2427 …clEnv->library->clEnqueueMapBuffer(queue, histogramBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, l… in ComputeEqualizeImage()
2432 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, histogramBuffer, CL_TRUE, 0, length * sizeof… in ComputeEqualizeImage()
2443 …clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, histogramBuffer, histogram, 0, NULL, NUL… in ComputeEqualizeImage()
2454 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeEqualizeImage()
2574 …imageBuffer = clEnv->library->clCreateBuffer(context, mem_flags, length * sizeof(CLPixelPacket), (… in ComputeEqualizeImage()
2595 …equalizeMapBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(Pix… in ComputeEqualizeImage()
2612 clStatus=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeEqualizeImage()
2613 …clStatus|=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(ChannelType),&image->channel_ma… in ComputeEqualizeImage()
2614 …clStatus|=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(cl_mem),(void *)&equalizeMapBuf… in ComputeEqualizeImage()
2615 clStatus|=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(cl_float4),&white); in ComputeEqualizeImage()
2616 clStatus|=clEnv->library->clSetKernelArg(equalizeKernel,i++,sizeof(cl_float4),&black); in ComputeEqualizeImage()
2627 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, equalizeKernel, 2, NULL, global_work_size… in ComputeEqualizeImage()
2640 …clEnv->library->clEnqueueMapBuffer(queue, imageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, lengt… in ComputeEqualizeImage()
2645 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, imageBuffer, CL_TRUE, 0, length * sizeof(CLP… in ComputeEqualizeImage()
2660 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeEqualizeImage()
2664 clEnv->library->clReleaseMemObject(equalizeMapBuffer); in ComputeEqualizeImage()
2668 clEnv->library->clReleaseMemObject(histogramBuffer); in ComputeEqualizeImage()
2690 clEnv; in AccelerateEqualizeImage() local
2701 clEnv=getOpenCLEnvironment(exception); in AccelerateEqualizeImage()
2702 if (clEnv == (MagickCLEnv) NULL) in AccelerateEqualizeImage()
2705 status=ComputeEqualizeImage(image,clEnv,exception); in AccelerateEqualizeImage()
2721 static MagickBooleanType ComputeFunctionImage(Image *image,MagickCLEnv clEnv, in ComputeFunctionImage() argument
2765 device=RequestOpenCLDevice(clEnv); in ComputeFunctionImage()
2842 clEnv; in AccelerateFunctionImage() local
2852 clEnv=getOpenCLEnvironment(exception); in AccelerateFunctionImage()
2853 if (clEnv == (MagickCLEnv) NULL) in AccelerateFunctionImage()
2856 status=ComputeFunctionImage(image,clEnv,function,number_parameters, in AccelerateFunctionImage()
2873 static MagickBooleanType ComputeGrayscaleImage(Image *image,MagickCLEnv clEnv, in ComputeGrayscaleImage() argument
2912 device=RequestOpenCLDevice(clEnv); in ComputeGrayscaleImage()
2969 clEnv; in AccelerateGrayscaleImage() local
2988 clEnv=getOpenCLEnvironment(exception); in AccelerateGrayscaleImage()
2989 if (clEnv == (MagickCLEnv) NULL) in AccelerateGrayscaleImage()
2992 status=ComputeGrayscaleImage(image,clEnv,method,exception); in AccelerateGrayscaleImage()
3008 static Image *ComputeLocalContrastImage(const Image *image,MagickCLEnv clEnv, in ComputeLocalContrastImage() argument
3074 device = RequestOpenCLDevice(clEnv); in ComputeLocalContrastImage()
3100 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeLocalContrastImage()
3138 …filteredImageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(C… in ComputeLocalContrastImage()
3150 …tempImageBuffer = clEnv->library->clCreateBuffer(device->context, CL_MEM_READ_WRITE, length * size… in ComputeLocalContrastImage()
3185 … clStatus=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeLocalContrastImage()
3186 …clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(cl_mem),(void *)&filteredImageBu… in ComputeLocalContrastImage()
3187 …clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(cl_mem),(void *)&tempImageBuffer… in ComputeLocalContrastImage()
3188 clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(cl_int),(void *)&iRadius); in ComputeLocalContrastImage()
3189 …clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(unsigned int),(void *)&imageColu… in ComputeLocalContrastImage()
3190 …clStatus|=clEnv->library->clSetKernelArg(blurRowKernel,i++,sizeof(unsigned int),(void *)&imageRows… in ComputeLocalContrastImage()
3214 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, blurRowKernel, 2, goffset, gsize, wsize, … in ComputeLocalContrastImage()
3220 clEnv->library->clFlush(queue); in ComputeLocalContrastImage()
3228 … clStatus=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeLocalContrastImage()
3229 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(cl_mem),(void *)&filteredImag… in ComputeLocalContrastImage()
3230 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(cl_mem),(void *)&tempImageBuf… in ComputeLocalContrastImage()
3231 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(unsigned int),(void *)&iRadiu… in ComputeLocalContrastImage()
3232 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(cl_float),(void *)&FStrength); in ComputeLocalContrastImage()
3233 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(unsigned int),(void *)&imageC… in ComputeLocalContrastImage()
3234 …clStatus|=clEnv->library->clSetKernelArg(blurColumnKernel,i++,sizeof(unsigned int),(void *)&imageR… in ComputeLocalContrastImage()
3258 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, blurColumnKernel, 2, goffset, gsize, wsiz… in ComputeLocalContrastImage()
3264 clEnv->library->clFlush(queue); in ComputeLocalContrastImage()
3274 …clEnv->library->clEnqueueMapBuffer(queue, filteredImageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, … in ComputeLocalContrastImage()
3279 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, filteredImageBuffer, CL_TRUE, 0, length * si… in ComputeLocalContrastImage()
3296 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeLocalContrastImage()
3298 clEnv->library->clReleaseMemObject(filteredImageBuffer); in ComputeLocalContrastImage()
3300 clEnv->library->clReleaseMemObject(tempImageBuffer); in ComputeLocalContrastImage()
3302 clEnv->library->clReleaseMemObject(imageKernelBuffer); in ComputeLocalContrastImage()
3330 clEnv; in AccelerateLocalContrastImage() local
3338 clEnv=getOpenCLEnvironment(exception); in AccelerateLocalContrastImage()
3339 if (clEnv == (MagickCLEnv) NULL) in AccelerateLocalContrastImage()
3342 filteredImage=ComputeLocalContrastImage(image,clEnv,radius,strength, in AccelerateLocalContrastImage()
3359 static MagickBooleanType ComputeModulateImage(Image *image,MagickCLEnv clEnv, in ComputeModulateImage() argument
3418 device = RequestOpenCLDevice(clEnv); in ComputeModulateImage()
3449 …imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, length * sizeof(CLPixelPa… in ComputeModulateImage()
3469 clStatus=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_mem),(void *)&imageBuffer); in ComputeModulateImage()
3470 clStatus|=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_float),&bright); in ComputeModulateImage()
3471 clStatus|=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_float),&hue); in ComputeModulateImage()
3472 clStatus|=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_float),&saturation); in ComputeModulateImage()
3473 clStatus|=clEnv->library->clSetKernelArg(modulateKernel,i++,sizeof(cl_float),&color); in ComputeModulateImage()
3485 …clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, modulateKernel, 2, NULL, global_work_size… in ComputeModulateImage()
3497 …clEnv->library->clEnqueueMapBuffer(queue, imageBuffer, CL_TRUE, CL_MAP_READ|CL_MAP_WRITE, 0, lengt… in ComputeModulateImage()
3502 …clStatus = clEnv->library->clEnqueueReadBuffer(queue, imageBuffer, CL_TRUE, 0, length * sizeof(CLP… in ComputeModulateImage()
3517 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeModulateImage()
3538 clEnv; in AccelerateModulateImage() local
3551 clEnv=getOpenCLEnvironment(exception); in AccelerateModulateImage()
3552 if (clEnv == (MagickCLEnv) NULL) in AccelerateModulateImage()
3555 status=ComputeModulateImage(image,clEnv,percent_brightness,percent_hue, in AccelerateModulateImage()
3572 static Image* ComputeMotionBlurImage(const Image *image,MagickCLEnv clEnv, in ComputeMotionBlurImage() argument
3656 device = RequestOpenCLDevice(clEnv); in ComputeMotionBlurImage()
3687 imageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, in ComputeMotionBlurImage()
3729 filteredImageBuffer = clEnv->library->clCreateBuffer(device->context, mem_flags, in ComputeMotionBlurImage()
3739 imageKernelBuffer = clEnv->library->clCreateBuffer(device->context, in ComputeMotionBlurImage()
3750 kernelBufferPtr = (float*)clEnv->library->clEnqueueMapBuffer(queue, imageKernelBuffer, in ComputeMotionBlurImage()
3762 clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, imageKernelBuffer, kernelBufferPtr, in ComputeMotionBlurImage()
3771 offsetBuffer = clEnv->library->clCreateBuffer(device->context, in ComputeMotionBlurImage()
3781 offsetBufferPtr = (int*)clEnv->library->clEnqueueMapBuffer(queue, offsetBuffer, CL_TRUE, in ComputeMotionBlurImage()
3794 clStatus = clEnv->library->clEnqueueUnmapMemObject(queue, offsetBuffer, offsetBufferPtr, 0, in ComputeMotionBlurImage()
3819 clStatus=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_mem), in ComputeMotionBlurImage()
3821 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_mem), in ComputeMotionBlurImage()
3825 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(unsigned int), in ComputeMotionBlurImage()
3827 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(unsigned int), in ComputeMotionBlurImage()
3829 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_mem), in ComputeMotionBlurImage()
3831 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(unsigned int), in ComputeMotionBlurImage()
3833 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_mem), in ComputeMotionBlurImage()
3841 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(cl_float4), &biasPixel); in ComputeMotionBlurImage()
3843 …clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(ChannelType), &image->channel… in ComputeMotionBlurImage()
3845 clStatus|=clEnv->library->clSetKernelArg(motionBlurKernel,i++,sizeof(unsigned int), &matte); in ComputeMotionBlurImage()
3862 clStatus = clEnv->library->clEnqueueNDRangeKernel(queue, motionBlurKernel, 2, NULL, in ComputeMotionBlurImage()
3876 clEnv->library->clEnqueueMapBuffer(queue, filteredImageBuffer, CL_TRUE, in ComputeMotionBlurImage()
3883 clStatus = clEnv->library->clEnqueueReadBuffer(queue, filteredImageBuffer, CL_TRUE, 0, in ComputeMotionBlurImage()
3901 clEnv->library->clReleaseMemObject(filteredImageBuffer); in ComputeMotionBlurImage()
3903 clEnv->library->clReleaseMemObject(imageBuffer); in ComputeMotionBlurImage()
3905 clEnv->library->clReleaseMemObject(imageKernelBuffer); in ComputeMotionBlurImage()
3926 clEnv; in AccelerateMotionBlurImage() local
3936 clEnv=getOpenCLEnvironment(exception); in AccelerateMotionBlurImage()
3937 if (clEnv == (MagickCLEnv) NULL) in AccelerateMotionBlurImage()
3940 filteredImage=ComputeMotionBlurImage(image,clEnv,kernel,width,offset, in AccelerateMotionBlurImage()
4314 static Image *ComputeResizeImage(const Image* image,MagickCLEnv clEnv, in ComputeResizeImage() argument
4360 device=RequestOpenCLDevice(clEnv); in ComputeResizeImage()
4491 clEnv; in AccelerateResizeImage() local
4505 clEnv=getOpenCLEnvironment(exception); in AccelerateResizeImage()
4506 if (clEnv == (MagickCLEnv) NULL) in AccelerateResizeImage()
4509 filteredImage=ComputeResizeImage(image,clEnv,resizedColumns,resizedRows, in AccelerateResizeImage()
4526 static Image* ComputeRotationalBlurImage(const Image *image,MagickCLEnv clEnv, in ComputeRotationalBlurImage() argument
4584 device=RequestOpenCLDevice(clEnv); in ComputeRotationalBlurImage()
4696 clEnv; in AccelerateRotationalBlurImage() local
4706 clEnv=getOpenCLEnvironment(exception); in AccelerateRotationalBlurImage()
4707 if (clEnv == (MagickCLEnv) NULL) in AccelerateRotationalBlurImage()
4710 filteredImage=ComputeRotationalBlurImage(image,clEnv,angle,exception); in AccelerateRotationalBlurImage()
4726 static Image *ComputeUnsharpMaskImage(const Image *image,MagickCLEnv clEnv, in ComputeUnsharpMaskImage() argument
4785 device=RequestOpenCLDevice(clEnv); in ComputeUnsharpMaskImage()
4918 MagickCLEnv clEnv,const double radius,const double sigma,const double gain, in ComputeUnsharpMaskImageSingle() argument
4966 device=RequestOpenCLDevice(clEnv); in ComputeUnsharpMaskImageSingle()
5051 clEnv; in AccelerateUnsharpMaskImage() local
5059 clEnv=getOpenCLEnvironment(exception); in AccelerateUnsharpMaskImage()
5060 if (clEnv == (MagickCLEnv) NULL) in AccelerateUnsharpMaskImage()
5064 filteredImage=ComputeUnsharpMaskImageSingle(image,clEnv,radius,sigma,gain, in AccelerateUnsharpMaskImage()
5067 filteredImage=ComputeUnsharpMaskImage(image,clEnv,radius,sigma,gain, in AccelerateUnsharpMaskImage()
5072 static Image *ComputeWaveletDenoiseImage(const Image *image,MagickCLEnv clEnv, in ComputeWaveletDenoiseImage() argument
5129 device=RequestOpenCLDevice(clEnv); in ComputeWaveletDenoiseImage()
5221 clEnv; in AccelerateWaveletDenoiseImage() local
5229 clEnv=getOpenCLEnvironment(exception); in AccelerateWaveletDenoiseImage()
5230 if (clEnv == (MagickCLEnv) NULL) in AccelerateWaveletDenoiseImage()
5233 filteredImage=ComputeWaveletDenoiseImage(image,clEnv,threshold,exception); in AccelerateWaveletDenoiseImage()