59 ctx->command_queue = clCreateCommandQueue(
60 ctx->ocf.hwctx->context,
61 ctx->ocf.hwctx->device_id,
68 if (
ctx->blend > 0.0001) {
69 ctx->kernel_colorkey = clCreateKernel(
ctx->ocf.program,
"colorkey_blend", &cle);
72 ctx->kernel_colorkey = clCreateKernel(
ctx->ocf.program,
"colorkey", &cle);
76 for (
int i = 0;
i < 4; ++
i) {
77 ctx->colorkey_rgba_float.s[
i] = (float)
ctx->colorkey_rgba[
i] / 255.0;
84 if (
ctx->command_queue)
85 clReleaseCommandQueue(
ctx->command_queue);
86 if (
ctx->kernel_colorkey)
87 clReleaseKernel(
ctx->kernel_colorkey);
99 size_t global_work[2];
127 src = (cl_mem)input_frame->
data[0];
139 if (colorkey_ctx->
blend > 0.0001) {
147 cle = clEnqueueNDRangeKernel(
185 if (
ctx->kernel_colorkey) {
186 cle = clReleaseKernel(
ctx->kernel_colorkey);
187 if (cle != CL_SUCCESS)
189 "kernel: %d.\n", cle);
192 if (
ctx->command_queue) {
193 cle = clReleaseCommandQueue(
ctx->command_queue);
194 if (cle != CL_SUCCESS)
196 "command queue: %d.\n", cle);
221 #define OFFSET(x) offsetof(ColorkeyOpenCLContext, x)
222 #define FLAGS AV_OPT_FLAG_FILTERING_PARAM|AV_OPT_FLAG_VIDEO_PARAM
234 .
name =
"colorkey_opencl",
235 .description =
NULL_IF_CONFIG_SMALL(
"Turns a certain color into transparency. Operates on RGB colors."),
237 .priv_class = &colorkey_opencl_class,
static int query_formats(AVFilterContext *ctx)
static const AVFilterPad inputs[]
static const AVFilterPad outputs[]
int ff_filter_frame(AVFilterLink *link, AVFrame *frame)
Send a frame of data to the next filter.
Main libavfilter public API header.
static av_cold int init(AVCodecContext *avctx)
const char * ff_opencl_source_colorkey
static av_cold int uninit(AVCodecContext *avctx)
void av_frame_free(AVFrame **frame)
Free the frame and any dynamically allocated objects in it, e.g.
int av_frame_copy_props(AVFrame *dst, const AVFrame *src)
Copy only "metadata" fields from src to dst.
#define AV_LOG_ERROR
Something went wrong and cannot losslessly be recovered.
static int output_frame(H264Context *h, AVFrame *dst, H264Picture *srcp)
#define FF_FILTER_FLAG_HWFRAME_AWARE
The filter is aware of hardware frames, and any hardware frame context should not be automatically pr...
common internal API header
#define NULL_IF_CONFIG_SMALL(x)
Return NULL if CONFIG_SMALL is true, otherwise the argument without modification.
void ff_opencl_filter_uninit(AVFilterContext *avctx)
Uninitialise an OpenCL filter context.
int ff_opencl_filter_load_program(AVFilterContext *avctx, const char **program_source_array, int nb_strings)
Load a new OpenCL program from strings in memory.
int ff_opencl_filter_config_input(AVFilterLink *inlink)
Check that the input link contains a suitable hardware frames context and extract the device from it.
int ff_opencl_filter_init(AVFilterContext *avctx)
Initialise an OpenCL filter context.
int ff_opencl_filter_work_size_from_image(AVFilterContext *avctx, size_t *work_size, AVFrame *frame, int plane, int block_alignment)
Find the work size needed needed for a given plane of an image.
int ff_opencl_filter_config_output(AVFilterLink *outlink)
Create a suitable hardware frames context for the output.
int ff_opencl_filter_query_formats(AVFilterContext *avctx)
Return that all inputs and outputs support only AV_PIX_FMT_OPENCL.
#define CL_SET_KERNEL_ARG(kernel, arg_num, type, arg)
set argument to specific Kernel.
#define CL_FAIL_ON_ERROR(errcode,...)
A helper macro to handle OpenCL errors.
@ AV_PIX_FMT_ARGB
packed ARGB 8:8:8:8, 32bpp, ARGBARGB...
@ AV_PIX_FMT_BGRA
packed BGRA 8:8:8:8, 32bpp, BGRABGRA...
@ AV_PIX_FMT_ABGR
packed ABGR 8:8:8:8, 32bpp, ABGRABGR...
@ AV_PIX_FMT_RGBA
packed RGBA 8:8:8:8, 32bpp, RGBARGBA...
uint8_t * data
The data buffer.
void * priv
private data for use by the filter
AVFilterLink ** outputs
array of pointers to output links
A link between two filters.
int w
agreed upon image width
int h
agreed upon image height
AVFilterContext * dst
dest filter
A filter pad used for either input or output.
const char * name
Pad name.
const char * name
Filter name.
This structure describes decoded (raw) audio or video data.
uint8_t * data[AV_NUM_DATA_POINTERS]
pointer to the picture/channel planes.
AVBufferRef * hw_frames_ctx
For hwaccel-format frames, this should be a reference to the AVHWFramesContext describing the frame.
This struct describes a set or pool of "hardware" frames (i.e.
enum AVPixelFormat sw_format
The pixel format identifying the actual data layout of the hardware frames.
cl_float4 colorkey_rgba_float
cl_kernel kernel_colorkey
cl_command_queue command_queue
static av_cold void colorkey_opencl_uninit(AVFilterContext *avctx)
static const AVOption colorkey_opencl_options[]
AVFILTER_DEFINE_CLASS(colorkey_opencl)
static int filter_frame(AVFilterLink *link, AVFrame *input_frame)
AVFilter ff_vf_colorkey_opencl
static const AVFilterPad colorkey_opencl_inputs[]
static const AVFilterPad colorkey_opencl_outputs[]
static int colorkey_opencl_init(AVFilterContext *avctx)
AVFrame * ff_get_video_buffer(AVFilterLink *link, int w, int h)
Request a picture buffer with a specific set of permissions.