FFmpeg
nvenc.c
Go to the documentation of this file.
1 /*
2  * H.264/HEVC/AV1 hardware encoding using nvidia nvenc
3  * Copyright (c) 2016 Timo Rothenpieler <timo@rothenpieler.org>
4  *
5  * This file is part of FFmpeg.
6  *
7  * FFmpeg is free software; you can redistribute it and/or
8  * modify it under the terms of the GNU Lesser General Public
9  * License as published by the Free Software Foundation; either
10  * version 2.1 of the License, or (at your option) any later version.
11  *
12  * FFmpeg is distributed in the hope that it will be useful,
13  * but WITHOUT ANY WARRANTY; without even the implied warranty of
14  * MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the GNU
15  * Lesser General Public License for more details.
16  *
17  * You should have received a copy of the GNU Lesser General Public
18  * License along with FFmpeg; if not, write to the Free Software
19  * Foundation, Inc., 51 Franklin Street, Fifth Floor, Boston, MA 02110-1301 USA
20  */
21 
22 #include "config.h"
23 #include "config_components.h"
24 
25 #include "nvenc.h"
26 #include "hevc/sei.h"
27 #if CONFIG_AV1_NVENC_ENCODER
28 #include "av1.h"
29 #endif
30 
31 #include "libavutil/hwcontext_cuda.h"
32 #include "libavutil/hwcontext.h"
33 #include "libavutil/cuda_check.h"
34 #include "libavutil/imgutils.h"
35 #include "libavutil/mem.h"
36 #include "libavutil/pixdesc.h"
37 #include "libavutil/timecode_internal.h"
38 #include "libavutil/mathematics.h"
39 #include "libavutil/mastering_display_metadata.h"
40 #include "libavutil/stereo3d.h"
41 #include "libavutil/tdrdi.h"
42 #include "atsc_a53.h"
43 #include "codec_desc.h"
44 #include "encode.h"
45 #include "internal.h"
46 
47 #define CHECK_CU(x) FF_CUDA_CHECK_DL(avctx, dl_fn->cuda_dl, x)
48 
49 #define NVENC_CAP 0x30
50 
51 #ifndef NVENC_NO_DEPRECATED_RC
52 #define IS_CBR(rc) (rc == NV_ENC_PARAMS_RC_CBR || \
53  rc == NV_ENC_PARAMS_RC_CBR_LOWDELAY_HQ || \
54  rc == NV_ENC_PARAMS_RC_CBR_HQ)
55 #else
56 #define IS_CBR(rc) (rc == NV_ENC_PARAMS_RC_CBR)
57 #endif
58 
59 const enum AVPixelFormat ff_nvenc_pix_fmts[] = {
60  AV_PIX_FMT_YUV420P,
61  AV_PIX_FMT_NV12,
62  AV_PIX_FMT_P010,
63  AV_PIX_FMT_YUV444P,
64  AV_PIX_FMT_P016, // Truncated to 10bits
65 #ifdef NVENC_HAVE_422_SUPPORT
66  AV_PIX_FMT_NV16,
67  AV_PIX_FMT_P210,
68  AV_PIX_FMT_P216,
69 #endif
70  AV_PIX_FMT_YUV444P10MSB,
71  AV_PIX_FMT_YUV444P16, // Truncated to 10bits
72  AV_PIX_FMT_0RGB32,
73  AV_PIX_FMT_RGB32,
74  AV_PIX_FMT_0BGR32,
75  AV_PIX_FMT_BGR32,
76  AV_PIX_FMT_X2RGB10,
77  AV_PIX_FMT_X2BGR10,
78  AV_PIX_FMT_GBRP,
79  AV_PIX_FMT_GBRP10MSB,
80  AV_PIX_FMT_GBRP16, // Truncated to 10bits
81  AV_PIX_FMT_CUDA,
82 #if CONFIG_D3D11VA
83  AV_PIX_FMT_D3D11,
84 #endif
85  AV_PIX_FMT_NONE
86 };
87 
88 const AVCodecHWConfigInternal *const ff_nvenc_hw_configs[] = {
89  HW_CONFIG_ENCODER_FRAMES(CUDA, CUDA),
90  HW_CONFIG_ENCODER_DEVICE(NONE, CUDA),
91 #if CONFIG_D3D11VA
92  HW_CONFIG_ENCODER_FRAMES(D3D11, D3D11VA),
93  HW_CONFIG_ENCODER_DEVICE(NONE, D3D11VA),
94 #endif
95  NULL,
96 };
97 
98 #define IS_10BIT(pix_fmt) (pix_fmt == AV_PIX_FMT_P010 || \
99  pix_fmt == AV_PIX_FMT_P016 || \
100  pix_fmt == AV_PIX_FMT_P210 || \
101  pix_fmt == AV_PIX_FMT_P216 || \
102  pix_fmt == AV_PIX_FMT_YUV444P10MSB || \
103  pix_fmt == AV_PIX_FMT_YUV444P16 || \
104  pix_fmt == AV_PIX_FMT_X2RGB10 || \
105  pix_fmt == AV_PIX_FMT_X2BGR10 || \
106  pix_fmt == AV_PIX_FMT_GBRP10MSB || \
107  pix_fmt == AV_PIX_FMT_GBRP16)
108 
109 #define IS_RGB(pix_fmt) (pix_fmt == AV_PIX_FMT_0RGB32 || \
110  pix_fmt == AV_PIX_FMT_RGB32 || \
111  pix_fmt == AV_PIX_FMT_0BGR32 || \
112  pix_fmt == AV_PIX_FMT_BGR32 || \
113  pix_fmt == AV_PIX_FMT_X2RGB10 || \
114  pix_fmt == AV_PIX_FMT_X2BGR10)
115 
116 #define IS_YUV444(pix_fmt) (pix_fmt == AV_PIX_FMT_YUV444P || \
117  pix_fmt == AV_PIX_FMT_YUV444P10MSB || \
118  pix_fmt == AV_PIX_FMT_YUV444P16 || \
119  pix_fmt == AV_PIX_FMT_GBRP || \
120  pix_fmt == AV_PIX_FMT_GBRP10MSB || \
121  pix_fmt == AV_PIX_FMT_GBRP16 || \
122  (ctx->rgb_mode == NVENC_RGB_MODE_444 && IS_RGB(pix_fmt)))
123 
124 #define IS_YUV422(pix_fmt) (pix_fmt == AV_PIX_FMT_NV16 || \
125  pix_fmt == AV_PIX_FMT_P210 || \
126  pix_fmt == AV_PIX_FMT_P216)
127 
128 #define IS_GBRP(pix_fmt) (pix_fmt == AV_PIX_FMT_GBRP || \
129  pix_fmt == AV_PIX_FMT_GBRP10MSB || \
130  pix_fmt == AV_PIX_FMT_GBRP16)
131 
132 static const struct {
133  NVENCSTATUS nverr;
134  int averr;
135  const char *desc;
136 } nvenc_errors[] = {
137  { NV_ENC_SUCCESS, 0, "success" },
138  { NV_ENC_ERR_NO_ENCODE_DEVICE, AVERROR(ENOENT), "no encode device" },
139  { NV_ENC_ERR_UNSUPPORTED_DEVICE, AVERROR(ENOSYS), "unsupported device" },
140  { NV_ENC_ERR_INVALID_ENCODERDEVICE, AVERROR(EINVAL), "invalid encoder device" },
141  { NV_ENC_ERR_INVALID_DEVICE, AVERROR(EINVAL), "invalid device" },
142  { NV_ENC_ERR_DEVICE_NOT_EXIST, AVERROR(EIO), "device does not exist" },
143  { NV_ENC_ERR_INVALID_PTR, AVERROR(EFAULT), "invalid ptr" },
144  { NV_ENC_ERR_INVALID_EVENT, AVERROR(EINVAL), "invalid event" },
145  { NV_ENC_ERR_INVALID_PARAM, AVERROR(EINVAL), "invalid param" },
146  { NV_ENC_ERR_INVALID_CALL, AVERROR(EINVAL), "invalid call" },
147  { NV_ENC_ERR_OUT_OF_MEMORY, AVERROR(ENOMEM), "out of memory" },
148  { NV_ENC_ERR_ENCODER_NOT_INITIALIZED, AVERROR(EINVAL), "encoder not initialized" },
149  { NV_ENC_ERR_UNSUPPORTED_PARAM, AVERROR(ENOSYS), "unsupported param" },
150  { NV_ENC_ERR_LOCK_BUSY, AVERROR(EAGAIN), "lock busy" },
151  { NV_ENC_ERR_NOT_ENOUGH_BUFFER, AVERROR_BUFFER_TOO_SMALL, "not enough buffer"},
152  { NV_ENC_ERR_INVALID_VERSION, AVERROR(EINVAL), "invalid version" },
153  { NV_ENC_ERR_MAP_FAILED, AVERROR(EIO), "map failed" },
154  { NV_ENC_ERR_NEED_MORE_INPUT, AVERROR(EAGAIN), "need more input" },
155  { NV_ENC_ERR_ENCODER_BUSY, AVERROR(EAGAIN), "encoder busy" },
156  { NV_ENC_ERR_EVENT_NOT_REGISTERD, AVERROR(EBADF), "event not registered" },
157  { NV_ENC_ERR_GENERIC, AVERROR_UNKNOWN, "generic error" },
158  { NV_ENC_ERR_INCOMPATIBLE_CLIENT_KEY, AVERROR(EINVAL), "incompatible client key" },
159  { NV_ENC_ERR_UNIMPLEMENTED, AVERROR(ENOSYS), "unimplemented" },
160  { NV_ENC_ERR_RESOURCE_REGISTER_FAILED, AVERROR(EIO), "resource register failed" },
161  { NV_ENC_ERR_RESOURCE_NOT_REGISTERED, AVERROR(EBADF), "resource not registered" },
162  { NV_ENC_ERR_RESOURCE_NOT_MAPPED, AVERROR(EBADF), "resource not mapped" },
163 };
164 
165 static int nvenc_map_error(NVENCSTATUS err, const char **desc)
166 {
167  int i;
168  for (i = 0; i < FF_ARRAY_ELEMS(nvenc_errors); i++) {
169  if (nvenc_errors[i].nverr == err) {
170  if (desc)
171  *desc = nvenc_errors[i].desc;
172  return nvenc_errors[i].averr;
173  }
174  }
175  if (desc)
176  *desc = "unknown error";
177  return AVERROR_UNKNOWN;
178 }
179 
180 static int nvenc_print_error(AVCodecContext *avctx, NVENCSTATUS err,
181  const char *error_string)
182 {
183  const char *desc;
184  const char *details = "(no details)";
185  int ret = nvenc_map_error(err, &desc);
186 
187 #ifdef NVENC_HAVE_GETLASTERRORSTRING
188  NvencContext *ctx = avctx->priv_data;
189  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &ctx->nvenc_dload_funcs.nvenc_funcs;
190 
191  if (p_nvenc && ctx->nvencoder)
192  details = p_nvenc->nvEncGetLastErrorString(ctx->nvencoder);
193 #endif
194 
195  av_log(avctx, AV_LOG_ERROR, "%s: %s (%d): %s\n", error_string, desc, err, details);
196 
197  return ret;
198 }
199 
200 typedef struct GUIDTuple {
201  const GUID guid;
202  int flags;
203 } GUIDTuple;
204 
205 #define PRESET_ALIAS(alias, name, ...) \
206  [PRESET_ ## alias] = { NV_ENC_PRESET_ ## name ## _GUID, __VA_ARGS__ }
207 
208 #define PRESET(name, ...) PRESET_ALIAS(name, name, __VA_ARGS__)
209 
210 static void nvenc_map_preset(NvencContext *ctx)
211 {
212  GUIDTuple presets[] = {
213 #ifdef NVENC_HAVE_NEW_PRESETS
214  PRESET(P1),
215  PRESET(P2),
216  PRESET(P3),
217  PRESET(P4),
218  PRESET(P5),
219  PRESET(P6),
220  PRESET(P7),
221  PRESET_ALIAS(SLOW, P7, NVENC_TWO_PASSES),
222  PRESET_ALIAS(MEDIUM, P4, NVENC_ONE_PASS),
223  PRESET_ALIAS(FAST, P1, NVENC_ONE_PASS),
224  // Compat aliases
225  PRESET_ALIAS(DEFAULT, P4, NVENC_DEPRECATED_PRESET),
226  PRESET_ALIAS(HP, P1, NVENC_DEPRECATED_PRESET),
227  PRESET_ALIAS(HQ, P7, NVENC_DEPRECATED_PRESET),
228  PRESET_ALIAS(BD, P5, NVENC_DEPRECATED_PRESET),
229  PRESET_ALIAS(LOW_LATENCY_DEFAULT, P4, NVENC_DEPRECATED_PRESET | NVENC_LOWLATENCY),
230  PRESET_ALIAS(LOW_LATENCY_HP, P1, NVENC_DEPRECATED_PRESET | NVENC_LOWLATENCY),
231  PRESET_ALIAS(LOW_LATENCY_HQ, P7, NVENC_DEPRECATED_PRESET | NVENC_LOWLATENCY),
232  PRESET_ALIAS(LOSSLESS_DEFAULT, P4, NVENC_DEPRECATED_PRESET | NVENC_LOSSLESS),
233  PRESET_ALIAS(LOSSLESS_HP, P1, NVENC_DEPRECATED_PRESET | NVENC_LOSSLESS),
234 #else
235  PRESET(DEFAULT),
236  PRESET(HP),
237  PRESET(HQ),
238  PRESET(BD),
239  PRESET_ALIAS(SLOW, HQ, NVENC_TWO_PASSES),
240  PRESET_ALIAS(MEDIUM, HQ, NVENC_ONE_PASS),
241  PRESET_ALIAS(FAST, HP, NVENC_ONE_PASS),
242  PRESET(LOW_LATENCY_DEFAULT, NVENC_LOWLATENCY),
243  PRESET(LOW_LATENCY_HP, NVENC_LOWLATENCY),
244  PRESET(LOW_LATENCY_HQ, NVENC_LOWLATENCY),
245  PRESET(LOSSLESS_DEFAULT, NVENC_LOSSLESS),
246  PRESET(LOSSLESS_HP, NVENC_LOSSLESS),
247 #endif
248  };
249 
250  GUIDTuple *t = &presets[ctx->preset];
251 
252  ctx->init_encode_params.presetGUID = t->guid;
253  ctx->flags = t->flags;
254 
255 #ifdef NVENC_HAVE_NEW_PRESETS
256  if (ctx->tuning_info == NV_ENC_TUNING_INFO_LOSSLESS)
257  ctx->flags |= NVENC_LOSSLESS;
258 #endif
259 }
260 
261 #undef PRESET
262 #undef PRESET_ALIAS
263 
264 static void nvenc_print_driver_requirement(AVCodecContext *avctx, int level)
265 {
266 #if NVENCAPI_CHECK_VERSION(13, 1)
267  const char *minver = "(unknown)";
268 #elif NVENCAPI_CHECK_VERSION(13, 0)
269  const char *minver = "570.0";
270 #elif NVENCAPI_CHECK_VERSION(12, 2)
271 # if defined(_WIN32) || defined(__CYGWIN__)
272  const char *minver = "551.76";
273 # else
274  const char *minver = "550.54.14";
275 # endif
276 #elif NVENCAPI_CHECK_VERSION(12, 1)
277 # if defined(_WIN32) || defined(__CYGWIN__)
278  const char *minver = "531.61";
279 # else
280  const char *minver = "530.41.03";
281 # endif
282 #elif NVENCAPI_CHECK_VERSION(12, 0)
283 # if defined(_WIN32) || defined(__CYGWIN__)
284  const char *minver = "522.25";
285 # else
286  const char *minver = "520.56.06";
287 # endif
288 #elif NVENCAPI_CHECK_VERSION(11, 1)
289 # if defined(_WIN32) || defined(__CYGWIN__)
290  const char *minver = "471.41";
291 # else
292  const char *minver = "470.57.02";
293 # endif
294 #elif NVENCAPI_CHECK_VERSION(11, 0)
295 # if defined(_WIN32) || defined(__CYGWIN__)
296  const char *minver = "456.71";
297 # else
298  const char *minver = "455.28";
299 # endif
300 #elif NVENCAPI_CHECK_VERSION(10, 0)
301 # if defined(_WIN32) || defined(__CYGWIN__)
302  const char *minver = "450.51";
303 # else
304  const char *minver = "445.87";
305 # endif
306 #elif NVENCAPI_CHECK_VERSION(9, 1)
307 # if defined(_WIN32) || defined(__CYGWIN__)
308  const char *minver = "436.15";
309 # else
310  const char *minver = "435.21";
311 # endif
312 #elif NVENCAPI_CHECK_VERSION(9, 0)
313 # if defined(_WIN32) || defined(__CYGWIN__)
314  const char *minver = "418.81";
315 # else
316  const char *minver = "418.30";
317 # endif
318 #elif NVENCAPI_CHECK_VERSION(8, 2)
319 # if defined(_WIN32) || defined(__CYGWIN__)
320  const char *minver = "397.93";
321 # else
322  const char *minver = "396.24";
323 #endif
324 #elif NVENCAPI_CHECK_VERSION(8, 1)
325 # if defined(_WIN32) || defined(__CYGWIN__)
326  const char *minver = "390.77";
327 # else
328  const char *minver = "390.25";
329 # endif
330 #else
331 # if defined(_WIN32) || defined(__CYGWIN__)
332  const char *minver = "378.66";
333 # else
334  const char *minver = "378.13";
335 # endif
336 #endif
337  av_log(avctx, level, "The minimum required Nvidia driver for nvenc is %s or newer\n", minver);
338 }
339 
340 #if NVENCAPI_CHECK_VERSION(12, 0)
341 #define to_nv_color_matrix(n) (NV_ENC_VUI_MATRIX_COEFFS)(n)
342 #define to_nv_color_pri(n) (NV_ENC_VUI_COLOR_PRIMARIES)(n)
343 #define to_nv_color_trc(n) (NV_ENC_VUI_TRANSFER_CHARACTERISTIC)(n)
344 #else
345 #define to_nv_color_matrix(n) (uint32_t)(n)
346 #define to_nv_color_pri(n) (uint32_t)(n)
347 #define to_nv_color_trc(n) (uint32_t)(n)
348 #endif
349 
350 static av_cold int nvenc_load_libraries(AVCodecContext *avctx)
351 {
352  NvencContext *ctx = avctx->priv_data;
353  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
354  NVENCSTATUS err;
355  uint32_t nvenc_max_ver;
356  int ret;
357 
358  ret = cuda_load_functions(&dl_fn->cuda_dl, avctx);
359  if (ret < 0)
360  return ret;
361 
362  ret = nvenc_load_functions(&dl_fn->nvenc_dl, avctx);
363  if (ret < 0) {
364  nvenc_print_driver_requirement(avctx, AV_LOG_ERROR);
365  return ret;
366  }
367 
368  err = dl_fn->nvenc_dl->NvEncodeAPIGetMaxSupportedVersion(&nvenc_max_ver);
369  if (err != NV_ENC_SUCCESS)
370  return nvenc_print_error(avctx, err, "Failed to query nvenc max version");
371 
372  av_log(avctx, AV_LOG_VERBOSE, "Loaded Nvenc version %d.%d\n", nvenc_max_ver >> 4, nvenc_max_ver & 0xf);
373 
374  if ((NVENCAPI_MAJOR_VERSION << 4 | NVENCAPI_MINOR_VERSION) > nvenc_max_ver) {
375  av_log(avctx, AV_LOG_ERROR, "Driver does not support the required nvenc API version. "
376  "Required: %d.%d Found: %d.%d\n",
377  NVENCAPI_MAJOR_VERSION, NVENCAPI_MINOR_VERSION,
378  nvenc_max_ver >> 4, nvenc_max_ver & 0xf);
379  nvenc_print_driver_requirement(avctx, AV_LOG_ERROR);
380  return AVERROR(ENOSYS);
381  }
382 
383  dl_fn->nvenc_funcs.version = NV_ENCODE_API_FUNCTION_LIST_VER;
384 
385  err = dl_fn->nvenc_dl->NvEncodeAPICreateInstance(&dl_fn->nvenc_funcs);
386  if (err != NV_ENC_SUCCESS)
387  return nvenc_print_error(avctx, err, "Failed to create nvenc instance");
388 
389  av_log(avctx, AV_LOG_VERBOSE, "Nvenc initialized successfully\n");
390 
391  return 0;
392 }
393 
394 static int nvenc_push_context(AVCodecContext *avctx)
395 {
396  NvencContext *ctx = avctx->priv_data;
397  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
398 
399  if (ctx->d3d11_device)
400  return 0;
401 
402  return CHECK_CU(dl_fn->cuda_dl->cuCtxPushCurrent(ctx->cu_context));
403 }
404 
405 static int nvenc_pop_context(AVCodecContext *avctx)
406 {
407  NvencContext *ctx = avctx->priv_data;
408  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
409  CUcontext dummy;
410 
411  if (ctx->d3d11_device)
412  return 0;
413 
414  return CHECK_CU(dl_fn->cuda_dl->cuCtxPopCurrent(&dummy));
415 }
416 
417 static av_cold int nvenc_open_session(AVCodecContext *avctx)
418 {
419  NV_ENC_OPEN_ENCODE_SESSION_EX_PARAMS params = { 0 };
420  NvencContext *ctx = avctx->priv_data;
421  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &ctx->nvenc_dload_funcs.nvenc_funcs;
422  NVENCSTATUS ret;
423 
424  params.version = NV_ENC_OPEN_ENCODE_SESSION_EX_PARAMS_VER;
425  params.apiVersion = NVENCAPI_VERSION;
426  if (ctx->d3d11_device) {
427  params.device = ctx->d3d11_device;
428  params.deviceType = NV_ENC_DEVICE_TYPE_DIRECTX;
429  } else {
430  params.device = ctx->cu_context;
431  params.deviceType = NV_ENC_DEVICE_TYPE_CUDA;
432  }
433 
434  ret = p_nvenc->nvEncOpenEncodeSessionEx(&params, &ctx->nvencoder);
435  if (ret != NV_ENC_SUCCESS) {
436  ctx->nvencoder = NULL;
437  return nvenc_print_error(avctx, ret, "OpenEncodeSessionEx failed");
438  }
439 
440  return 0;
441 }
442 
443 static int nvenc_check_codec_support(AVCodecContext *avctx)
444 {
445  NvencContext *ctx = avctx->priv_data;
446  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &ctx->nvenc_dload_funcs.nvenc_funcs;
447  int i, ret, count = 0;
448  GUID *guids = NULL;
449 
450  ret = p_nvenc->nvEncGetEncodeGUIDCount(ctx->nvencoder, &count);
451 
452  if (ret != NV_ENC_SUCCESS || !count)
453  return AVERROR(ENOSYS);
454 
455  guids = av_malloc(count * sizeof(GUID));
456  if (!guids)
457  return AVERROR(ENOMEM);
458 
459  ret = p_nvenc->nvEncGetEncodeGUIDs(ctx->nvencoder, guids, count, &count);
460  if (ret != NV_ENC_SUCCESS) {
461  ret = AVERROR(ENOSYS);
462  goto fail;
463  }
464 
465  ret = AVERROR(ENOSYS);
466  for (i = 0; i < count; i++) {
467  if (!memcmp(&guids[i], &ctx->init_encode_params.encodeGUID, sizeof(*guids))) {
468  ret = 0;
469  break;
470  }
471  }
472 
473 fail:
474  av_free(guids);
475 
476  return ret;
477 }
478 
479 static int nvenc_check_cap(AVCodecContext *avctx, NV_ENC_CAPS cap)
480 {
481  NvencContext *ctx = avctx->priv_data;
482  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &ctx->nvenc_dload_funcs.nvenc_funcs;
483  NV_ENC_CAPS_PARAM params = { 0 };
484  int ret, val = 0;
485 
486  params.version = NV_ENC_CAPS_PARAM_VER;
487  params.capsToQuery = cap;
488 
489  ret = p_nvenc->nvEncGetEncodeCaps(ctx->nvencoder, ctx->init_encode_params.encodeGUID, &params, &val);
490 
491  if (ret == NV_ENC_SUCCESS)
492  return val;
493  return 0;
494 }
495 
496 static int nvenc_check_capabilities(AVCodecContext *avctx)
497 {
498  NvencContext *ctx = avctx->priv_data;
499  int tmp, ret;
500 
501  ret = nvenc_check_codec_support(avctx);
502  if (ret < 0) {
503  av_log(avctx, AV_LOG_WARNING, "Codec not supported\n");
504  return ret;
505  }
506 
507  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_YUV444_ENCODE);
508  if (IS_YUV444(ctx->data_pix_fmt) && ret <= 0) {
509  av_log(avctx, AV_LOG_WARNING, "YUV444P not supported\n");
510  return AVERROR(ENOSYS);
511  }
512 
513 #ifdef NVENC_HAVE_422_SUPPORT
514  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_YUV422_ENCODE);
515 #else
516  ret = 0;
517 #endif
518  if (IS_YUV422(ctx->data_pix_fmt) && ret <= 0) {
519  av_log(avctx, AV_LOG_WARNING, "YUV422P not supported\n");
520  return AVERROR(ENOSYS);
521  }
522 
523  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_LOSSLESS_ENCODE);
524  if (ctx->flags & NVENC_LOSSLESS && ret <= 0) {
525  av_log(avctx, AV_LOG_WARNING, "Lossless encoding not supported\n");
526  return AVERROR(ENOSYS);
527  }
528 
529  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_WIDTH_MAX);
530  if (ret < avctx->width) {
531  av_log(avctx, AV_LOG_WARNING, "Width %d exceeds %d\n",
532  avctx->width, ret);
533  return AVERROR(ENOSYS);
534  }
535 
536  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_HEIGHT_MAX);
537  if (ret < avctx->height) {
538  av_log(avctx, AV_LOG_WARNING, "Height %d exceeds %d\n",
539  avctx->height, ret);
540  return AVERROR(ENOSYS);
541  }
542 
543  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_NUM_MAX_BFRAMES);
544  if (ret < avctx->max_b_frames) {
545  av_log(avctx, AV_LOG_WARNING, "Max B-frames %d exceed %d\n",
546  avctx->max_b_frames, ret);
547 
548  return AVERROR(ENOSYS);
549  }
550 
551  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_FIELD_ENCODING);
552  if (ret < 1 && avctx->flags & AV_CODEC_FLAG_INTERLACED_DCT) {
553  av_log(avctx, AV_LOG_WARNING,
554  "Interlaced encoding is not supported. Supported level: %d\n",
555  ret);
556  return AVERROR(ENOSYS);
557  }
558 
559  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_10BIT_ENCODE);
560  if ((IS_10BIT(ctx->data_pix_fmt) || ctx->highbitdepth) && ret <= 0) {
561  av_log(avctx, AV_LOG_WARNING, "10 bit encode not supported\n");
562  return AVERROR(ENOSYS);
563  }
564 
565  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_LOOKAHEAD);
566  if (ctx->rc_lookahead > 0 && ret <= 0) {
567  av_log(avctx, AV_LOG_WARNING, "RC lookahead not supported\n");
568  return AVERROR(ENOSYS);
569  }
570 
571  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_TEMPORAL_AQ);
572  if (ctx->temporal_aq > 0 && ret <= 0) {
573  av_log(avctx, AV_LOG_WARNING, "Temporal AQ not supported\n");
574  return AVERROR(ENOSYS);
575  }
576 
577  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_WEIGHTED_PREDICTION);
578  if (ctx->weighted_pred > 0 && ret <= 0) {
579  av_log (avctx, AV_LOG_WARNING, "Weighted Prediction not supported\n");
580  return AVERROR(ENOSYS);
581  }
582 
583  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_CABAC);
584  if (ctx->coder == NV_ENC_H264_ENTROPY_CODING_MODE_CABAC && ret <= 0) {
585  av_log(avctx, AV_LOG_WARNING, "CABAC entropy coding not supported\n");
586  return AVERROR(ENOSYS);
587  }
588 
589 #ifdef NVENC_HAVE_BFRAME_REF_MODE
590  tmp = (ctx->b_ref_mode >= 0) ? ctx->b_ref_mode : NV_ENC_BFRAME_REF_MODE_DISABLED;
591  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_BFRAME_REF_MODE);
592  if (tmp == NV_ENC_BFRAME_REF_MODE_EACH && ret != 1 && ret != 3) {
593  av_log(avctx, AV_LOG_WARNING, "Each B frame as reference is not supported\n");
594  return AVERROR(ENOSYS);
595  } else if (tmp != NV_ENC_BFRAME_REF_MODE_DISABLED && ret == 0) {
596  av_log(avctx, AV_LOG_WARNING, "B frames as references are not supported\n");
597  return AVERROR(ENOSYS);
598  }
599 #else
600  tmp = (ctx->b_ref_mode >= 0) ? ctx->b_ref_mode : 0;
601  if (tmp > 0) {
602  av_log(avctx, AV_LOG_WARNING, "B frames as references need SDK 8.1 at build time\n");
603  return AVERROR(ENOSYS);
604  }
605 #endif
606 
607 #ifdef NVENC_HAVE_MULTIPLE_REF_FRAMES
608  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_MULTIPLE_REF_FRAMES);
609  if(avctx->refs != NV_ENC_NUM_REF_FRAMES_AUTOSELECT && ret <= 0) {
610  av_log(avctx, AV_LOG_WARNING, "Multiple reference frames are not supported by the device\n");
611  return AVERROR(ENOSYS);
612  }
613 #else
614  if(avctx->refs != 0) {
615  av_log(avctx, AV_LOG_WARNING, "Multiple reference frames need SDK 9.1 at build time\n");
616  return AVERROR(ENOSYS);
617  }
618 #endif
619 
620 #ifdef NVENC_HAVE_SINGLE_SLICE_INTRA_REFRESH
621  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SINGLE_SLICE_INTRA_REFRESH);
622  if(ctx->single_slice_intra_refresh && ret <= 0) {
623  av_log(avctx, AV_LOG_WARNING, "Single slice intra refresh not supported by the device\n");
624  return AVERROR(ENOSYS);
625  }
626 #else
627  if(ctx->single_slice_intra_refresh) {
628  av_log(avctx, AV_LOG_WARNING, "Single slice intra refresh needs SDK 11.1 at build time\n");
629  return AVERROR(ENOSYS);
630  }
631 #endif
632 
633  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_INTRA_REFRESH);
634  if((ctx->intra_refresh || ctx->single_slice_intra_refresh) && ret <= 0) {
635  av_log(avctx, AV_LOG_WARNING, "Intra refresh not supported by the device\n");
636  return AVERROR(ENOSYS);
637  }
638 
639 #ifndef NVENC_HAVE_HEVC_CONSTRAINED_ENCODING
640  if (ctx->constrained_encoding && avctx->codec->id == AV_CODEC_ID_HEVC) {
641  av_log(avctx, AV_LOG_WARNING, "HEVC constrained encoding needs SDK 10.0 at build time\n");
642  return AVERROR(ENOSYS);
643  }
644 #endif
645 
646  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_CONSTRAINED_ENCODING);
647  if(ctx->constrained_encoding && ret <= 0) {
648  av_log(avctx, AV_LOG_WARNING, "Constrained encoding not supported by the device\n");
649  return AVERROR(ENOSYS);
650  }
651 
652 #if defined(NVENC_HAVE_TEMPORAL_FILTER) || defined(NVENC_HAVE_H264_AND_AV1_TEMPORAL_FILTER)
653  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_TEMPORAL_FILTER);
654  if(ctx->tf_level > 0 && ret <= 0) {
655  av_log(avctx, AV_LOG_WARNING, "Temporal filtering not supported by the device\n");
656  return AVERROR(ENOSYS);
657  }
658 #endif
659 
660 #ifdef NVENC_HAVE_LOOKAHEAD_LEVEL
661  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_LOOKAHEAD_LEVEL);
662  if(ctx->rc_lookahead > 0 && ctx->lookahead_level > 0 &&
663  ctx->lookahead_level != NV_ENC_LOOKAHEAD_LEVEL_AUTOSELECT &&
664  ctx->lookahead_level > ret)
665  {
666  av_log(avctx, AV_LOG_WARNING, "Lookahead level not supported. Maximum level: %d\n", ret);
667  return AVERROR(ENOSYS);
668  }
669 #endif
670 
671 #ifdef NVENC_HAVE_UNIDIR_B
672  ret = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_UNIDIRECTIONAL_B);
673  if(ctx->unidir_b && ret <= 0) {
674  av_log(avctx, AV_LOG_WARNING, "Unidirectional B-Frames not supported by the device\n");
675  return AVERROR(ENOSYS);
676  }
677 #endif
678 
679  ctx->support_dyn_bitrate = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_DYN_BITRATE_CHANGE);
680 
681 #ifdef NVENC_HAVE_MVHEVC
682  ctx->multiview_supported = nvenc_check_cap(avctx, NV_ENC_CAPS_SUPPORT_MVHEVC_ENCODE) > 0;
683  if (avctx->codec_id == AV_CODEC_ID_HEVC &&
684  ctx->profile == NV_ENC_HEVC_PROFILE_MULTIVIEW_MAIN &&
685  !ctx->multiview_supported) {
686  av_log(avctx, AV_LOG_WARNING, "Multiview not supported by the device\n");
687  return AVERROR(ENOSYS);
688  }
689 #endif
690 
691  return 0;
692 }
693 
694 static av_cold int nvenc_check_device(AVCodecContext *avctx, int idx)
695 {
696  NvencContext *ctx = avctx->priv_data;
697  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
698  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
699  char name[128] = { 0};
700  int major, minor, ret;
701  CUdevice cu_device;
702  int loglevel = AV_LOG_VERBOSE;
703 
704  if (ctx->device == LIST_DEVICES)
705  loglevel = AV_LOG_INFO;
706 
707  ret = CHECK_CU(dl_fn->cuda_dl->cuDeviceGet(&cu_device, idx));
708  if (ret < 0)
709  return ret;
710 
711  ret = CHECK_CU(dl_fn->cuda_dl->cuDeviceGetName(name, sizeof(name), cu_device));
712  if (ret < 0)
713  return ret;
714 
715  ret = CHECK_CU(dl_fn->cuda_dl->cuDeviceComputeCapability(&major, &minor, cu_device));
716  if (ret < 0)
717  return ret;
718 
719  av_log(avctx, loglevel, "[ GPU #%d - < %s > has Compute SM %d.%d ]\n", idx, name, major, minor);
720  if (((major << 4) | minor) < NVENC_CAP) {
721  av_log(avctx, loglevel, "does not support NVENC\n");
722  goto fail;
723  }
724 
725  if (ctx->device != idx && ctx->device != ANY_DEVICE)
726  return -1;
727 
728  ret = CHECK_CU(dl_fn->cuda_dl->cuCtxCreate(&ctx->cu_context_internal, 0, cu_device));
729  if (ret < 0)
730  goto fail;
731 
732  ctx->cu_context = ctx->cu_context_internal;
733  ctx->cu_stream = NULL;
734 
735  if ((ret = nvenc_pop_context(avctx)) < 0)
736  goto fail2;
737 
738  if ((ret = nvenc_open_session(avctx)) < 0)
739  goto fail2;
740 
741  if ((ret = nvenc_check_capabilities(avctx)) < 0)
742  goto fail3;
743 
744  av_log(avctx, loglevel, "supports NVENC\n");
745 
746  dl_fn->nvenc_device_count++;
747 
748  if (ctx->device == idx || ctx->device == ANY_DEVICE)
749  return 0;
750 
751 fail3:
752  if ((ret = nvenc_push_context(avctx)) < 0)
753  return ret;
754 
755  p_nvenc->nvEncDestroyEncoder(ctx->nvencoder);
756  ctx->nvencoder = NULL;
757 
758  if ((ret = nvenc_pop_context(avctx)) < 0)
759  return ret;
760 
761 fail2:
762  CHECK_CU(dl_fn->cuda_dl->cuCtxDestroy(ctx->cu_context_internal));
763  ctx->cu_context_internal = NULL;
764 
765 fail:
766  return AVERROR(ENOSYS);
767 }
768 
769 static av_cold int nvenc_setup_device(AVCodecContext *avctx)
770 {
771  NvencContext *ctx = avctx->priv_data;
772  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
773 
774  switch (avctx->codec->id) {
775  case AV_CODEC_ID_H264:
776  ctx->init_encode_params.encodeGUID = NV_ENC_CODEC_H264_GUID;
777  break;
778  case AV_CODEC_ID_HEVC:
779  ctx->init_encode_params.encodeGUID = NV_ENC_CODEC_HEVC_GUID;
780  break;
781 #if CONFIG_AV1_NVENC_ENCODER
782  case AV_CODEC_ID_AV1:
783  ctx->init_encode_params.encodeGUID = NV_ENC_CODEC_AV1_GUID;
784  break;
785 #endif
786  default:
787  return AVERROR_BUG;
788  }
789 
790  nvenc_map_preset(ctx);
791 
792  if (ctx->flags & NVENC_DEPRECATED_PRESET)
793  av_log(avctx, AV_LOG_WARNING, "The selected preset is deprecated. Use p1 to p7 + -tune or fast/medium/slow.\n");
794 
795  if (avctx->pix_fmt == AV_PIX_FMT_CUDA || avctx->pix_fmt == AV_PIX_FMT_D3D11 || avctx->hw_frames_ctx || avctx->hw_device_ctx) {
796  AVHWFramesContext *frames_ctx;
797  AVHWDeviceContext *hwdev_ctx;
798  AVCUDADeviceContext *cuda_device_hwctx = NULL;
799 #if CONFIG_D3D11VA
800  AVD3D11VADeviceContext *d3d11_device_hwctx = NULL;
801 #endif
802  int ret;
803 
804  if (avctx->hw_frames_ctx) {
805  frames_ctx = (AVHWFramesContext*)avctx->hw_frames_ctx->data;
806  if (frames_ctx->format == AV_PIX_FMT_CUDA)
807  cuda_device_hwctx = frames_ctx->device_ctx->hwctx;
808 #if CONFIG_D3D11VA
809  else if (frames_ctx->format == AV_PIX_FMT_D3D11)
810  d3d11_device_hwctx = frames_ctx->device_ctx->hwctx;
811 #endif
812  else
813  return AVERROR(EINVAL);
814  } else if (avctx->hw_device_ctx) {
815  hwdev_ctx = (AVHWDeviceContext*)avctx->hw_device_ctx->data;
816  if (hwdev_ctx->type == AV_HWDEVICE_TYPE_CUDA)
817  cuda_device_hwctx = hwdev_ctx->hwctx;
818 #if CONFIG_D3D11VA
819  else if (hwdev_ctx->type == AV_HWDEVICE_TYPE_D3D11VA)
820  d3d11_device_hwctx = hwdev_ctx->hwctx;
821 #endif
822  else
823  return AVERROR(EINVAL);
824  } else {
825  return AVERROR(EINVAL);
826  }
827 
828  if (cuda_device_hwctx) {
829  ctx->cu_context = cuda_device_hwctx->cuda_ctx;
830  ctx->cu_stream = cuda_device_hwctx->stream;
831  }
832 #if CONFIG_D3D11VA
833  else if (d3d11_device_hwctx) {
834  ctx->d3d11_device = d3d11_device_hwctx->device;
835  ID3D11Device_AddRef(ctx->d3d11_device);
836  }
837 #endif
838 
839  ret = nvenc_open_session(avctx);
840  if (ret < 0)
841  return ret;
842 
843  ret = nvenc_check_capabilities(avctx);
844  if (ret < 0) {
845  av_log(avctx, AV_LOG_FATAL, "Provided device doesn't support required NVENC features\n");
846  return ret;
847  }
848  } else {
849  int i, nb_devices = 0;
850 
851  if (CHECK_CU(dl_fn->cuda_dl->cuInit(0)) < 0)
852  return AVERROR_UNKNOWN;
853 
854  if (CHECK_CU(dl_fn->cuda_dl->cuDeviceGetCount(&nb_devices)) < 0)
855  return AVERROR_UNKNOWN;
856 
857  if (!nb_devices) {
858  av_log(avctx, AV_LOG_FATAL, "No CUDA capable devices found\n");
859  return AVERROR_EXTERNAL;
860  }
861 
862  av_log(avctx, AV_LOG_VERBOSE, "%d CUDA capable devices found\n", nb_devices);
863 
864  dl_fn->nvenc_device_count = 0;
865  for (i = 0; i < nb_devices; ++i) {
866  if ((nvenc_check_device(avctx, i)) >= 0 && ctx->device != LIST_DEVICES)
867  return 0;
868  }
869 
870  if (ctx->device == LIST_DEVICES)
871  return AVERROR_EXIT;
872 
873  if (!dl_fn->nvenc_device_count) {
874  av_log(avctx, AV_LOG_FATAL, "No capable devices found\n");
875  return AVERROR_EXTERNAL;
876  }
877 
878  av_log(avctx, AV_LOG_FATAL, "Requested GPU %d, but only %d GPUs are available!\n", ctx->device, nb_devices);
879  return AVERROR(EINVAL);
880  }
881 
882  return 0;
883 }
884 
885 static av_cold void set_constqp(AVCodecContext *avctx)
886 {
887  NvencContext *ctx = avctx->priv_data;
888  NV_ENC_RC_PARAMS *rc = &ctx->encode_config.rcParams;
889 #if CONFIG_AV1_NVENC_ENCODER
890  int qmax = avctx->codec->id == AV_CODEC_ID_AV1 ? 255 : 51;
891 #else
892  int qmax = 51;
893 #endif
894 
895  rc->rateControlMode = NV_ENC_PARAMS_RC_CONSTQP;
896 
897  if (ctx->init_qp_p >= 0) {
898  rc->constQP.qpInterP = ctx->init_qp_p;
899  if (ctx->init_qp_i >= 0 && ctx->init_qp_b >= 0) {
900  rc->constQP.qpIntra = ctx->init_qp_i;
901  rc->constQP.qpInterB = ctx->init_qp_b;
902  } else if (avctx->i_quant_factor != 0.0 && avctx->b_quant_factor != 0.0) {
903  rc->constQP.qpIntra = av_clip(
904  rc->constQP.qpInterP * fabs(avctx->i_quant_factor) + avctx->i_quant_offset + 0.5, 0, qmax);
905  rc->constQP.qpInterB = av_clip(
906  rc->constQP.qpInterP * fabs(avctx->b_quant_factor) + avctx->b_quant_offset + 0.5, 0, qmax);
907  } else {
908  rc->constQP.qpIntra = rc->constQP.qpInterP;
909  rc->constQP.qpInterB = rc->constQP.qpInterP;
910  }
911  } else if (ctx->cqp >= 0) {
912  rc->constQP.qpInterP = rc->constQP.qpInterB = rc->constQP.qpIntra = ctx->cqp;
913  if (avctx->b_quant_factor != 0.0)
914  rc->constQP.qpInterB = av_clip(ctx->cqp * fabs(avctx->b_quant_factor) + avctx->b_quant_offset + 0.5, 0, qmax);
915  if (avctx->i_quant_factor != 0.0)
916  rc->constQP.qpIntra = av_clip(ctx->cqp * fabs(avctx->i_quant_factor) + avctx->i_quant_offset + 0.5, 0, qmax);
917  }
918 
919  avctx->qmin = ctx->qmin = -1;
920  avctx->qmax = ctx->qmax = -1;
921 }
922 
923 static av_cold void set_vbr(AVCodecContext *avctx)
924 {
925  NvencContext *ctx = avctx->priv_data;
926  NV_ENC_RC_PARAMS *rc = &ctx->encode_config.rcParams;
927  int qp_inter_p;
928 #if CONFIG_AV1_NVENC_ENCODER
929  int qmax = avctx->codec->id == AV_CODEC_ID_AV1 ? 255 : 51;
930 #else
931  int qmax = 51;
932 #endif
933 
934  if (avctx->qmin >= 0 || avctx->qmax >= 0)
935  av_log(avctx, AV_LOG_WARNING, "Passing qmin/qmax via global AVCodecContext options. Use encoder options instead.\n");
936 
937  if (avctx->qmin >= 0 && ctx->qmin < 0)
938  ctx->qmin = avctx->qmin;
939  if (avctx->qmax >= 0 && ctx->qmax < 0)
940  ctx->qmax = avctx->qmax;
941  avctx->qmin = ctx->qmin;
942  avctx->qmax = ctx->qmax;
943 
944  if (ctx->qmin >= 0 && ctx->qmax >= 0) {
945  rc->enableMinQP = 1;
946  rc->enableMaxQP = 1;
947 
948  rc->minQP.qpInterB = ctx->qmin;
949  rc->minQP.qpInterP = ctx->qmin;
950  rc->minQP.qpIntra = ctx->qmin;
951 
952  rc->maxQP.qpInterB = ctx->qmax;
953  rc->maxQP.qpInterP = ctx->qmax;
954  rc->maxQP.qpIntra = ctx->qmax;
955 
956  qp_inter_p = (ctx->qmax + 3 * ctx->qmin) / 4; // biased towards Qmin
957  } else if (ctx->qmin >= 0) {
958  rc->enableMinQP = 1;
959 
960  rc->minQP.qpInterB = ctx->qmin;
961  rc->minQP.qpInterP = ctx->qmin;
962  rc->minQP.qpIntra = ctx->qmin;
963 
964  qp_inter_p = ctx->qmin;
965  } else {
966  qp_inter_p = 26; // default to 26
967  }
968 
969  rc->enableInitialRCQP = 1;
970 
971  if (ctx->init_qp_p < 0) {
972  rc->initialRCQP.qpInterP = qp_inter_p;
973  } else {
974  rc->initialRCQP.qpInterP = ctx->init_qp_p;
975  }
976 
977  if (ctx->init_qp_i < 0) {
978  if (avctx->i_quant_factor != 0.0 && avctx->b_quant_factor != 0.0) {
979  rc->initialRCQP.qpIntra = av_clip(
980  rc->initialRCQP.qpInterP * fabs(avctx->i_quant_factor) + avctx->i_quant_offset + 0.5, 0, qmax);
981  } else {
982  rc->initialRCQP.qpIntra = rc->initialRCQP.qpInterP;
983  }
984  } else {
985  rc->initialRCQP.qpIntra = ctx->init_qp_i;
986  }
987 
988  if (ctx->init_qp_b < 0) {
989  if (avctx->i_quant_factor != 0.0 && avctx->b_quant_factor != 0.0) {
990  rc->initialRCQP.qpInterB = av_clip(
991  rc->initialRCQP.qpInterP * fabs(avctx->b_quant_factor) + avctx->b_quant_offset + 0.5, 0, qmax);
992  } else {
993  rc->initialRCQP.qpInterB = rc->initialRCQP.qpInterP;
994  }
995  } else {
996  rc->initialRCQP.qpInterB = ctx->init_qp_b;
997  }
998 }
999 
1000 static av_cold void set_lossless(AVCodecContext *avctx)
1001 {
1002  NvencContext *ctx = avctx->priv_data;
1003  NV_ENC_RC_PARAMS *rc = &ctx->encode_config.rcParams;
1004 
1005  rc->rateControlMode = NV_ENC_PARAMS_RC_CONSTQP;
1006  rc->constQP.qpInterB = 0;
1007  rc->constQP.qpInterP = 0;
1008  rc->constQP.qpIntra = 0;
1009 
1010  avctx->qmin = ctx->qmin = -1;
1011  avctx->qmax = ctx->qmax = -1;
1012 }
1013 
1014 static void nvenc_override_rate_control(AVCodecContext *avctx)
1015 {
1016  NvencContext *ctx = avctx->priv_data;
1017  NV_ENC_RC_PARAMS *rc = &ctx->encode_config.rcParams;
1018 
1019  switch (ctx->rc) {
1020  case NV_ENC_PARAMS_RC_CONSTQP:
1021  set_constqp(avctx);
1022  return;
1023 #ifndef NVENC_NO_DEPRECATED_RC
1024  case NV_ENC_PARAMS_RC_VBR_MINQP:
1025  if (avctx->qmin < 0 && ctx->qmin < 0) {
1026  av_log(avctx, AV_LOG_WARNING,
1027  "The variable bitrate rate-control requires "
1028  "the 'qmin' option set.\n");
1029  set_vbr(avctx);
1030  return;
1031  }
1032  /* fall through */
1033  case NV_ENC_PARAMS_RC_VBR_HQ:
1034 #endif
1035  case NV_ENC_PARAMS_RC_VBR:
1036  set_vbr(avctx);
1037  break;
1038  case NV_ENC_PARAMS_RC_CBR:
1039 #ifndef NVENC_NO_DEPRECATED_RC
1040  case NV_ENC_PARAMS_RC_CBR_HQ:
1041  case NV_ENC_PARAMS_RC_CBR_LOWDELAY_HQ:
1042 #endif
1043  break;
1044  }
1045 
1046  rc->rateControlMode = ctx->rc;
1047 }
1048 
1049 static av_cold int nvenc_recalc_surfaces(AVCodecContext *avctx)
1050 {
1051  NvencContext *ctx = avctx->priv_data;
1052  // default minimum of 4 surfaces
1053  // multiply by 2 for number of NVENCs on gpu (hardcode to 2)
1054  // another multiply by 2 to avoid blocking next PBB group
1055  int nb_surfaces = FFMAX(4, ctx->encode_config.frameIntervalP * 2 * 2);
1056 
1057  // lookahead enabled
1058  if (ctx->rc_lookahead > 0) {
1059  // +1 is to account for lkd_bound calculation later
1060  // +4 is to allow sufficient pipelining with lookahead
1061  nb_surfaces = FFMAX(1, FFMAX(nb_surfaces, ctx->rc_lookahead + ctx->encode_config.frameIntervalP + 1 + 4));
1062  if (nb_surfaces > ctx->nb_surfaces && ctx->nb_surfaces > 0)
1063  {
1064  av_log(avctx, AV_LOG_WARNING,
1065  "Defined rc_lookahead requires more surfaces, "
1066  "increasing used surfaces %d -> %d\n", ctx->nb_surfaces, nb_surfaces);
1067  }
1068  ctx->nb_surfaces = FFMAX(nb_surfaces, ctx->nb_surfaces);
1069  } else {
1070  if (ctx->encode_config.frameIntervalP > 1 && ctx->nb_surfaces < nb_surfaces && ctx->nb_surfaces > 0)
1071  {
1072  av_log(avctx, AV_LOG_WARNING,
1073  "Defined b-frame requires more surfaces, "
1074  "increasing used surfaces %d -> %d\n", ctx->nb_surfaces, nb_surfaces);
1075  ctx->nb_surfaces = FFMAX(ctx->nb_surfaces, nb_surfaces);
1076  }
1077  else if (ctx->nb_surfaces <= 0)
1078  ctx->nb_surfaces = nb_surfaces;
1079  // otherwise use user specified value
1080  }
1081 
1082  ctx->nb_surfaces = FFMAX(1, FFMIN(MAX_REGISTERED_FRAMES, ctx->nb_surfaces));
1083  ctx->async_depth = FFMIN(ctx->async_depth, ctx->nb_surfaces - 1);
1084 
1085  // Output in the worst case will only start when the surface buffer is completely full.
1086  // Hence we need to keep at least the max amount of surfaces plus the max reorder delay around.
1087  ctx->frame_data_array_nb = FFMAX(ctx->nb_surfaces, ctx->nb_surfaces + ctx->encode_config.frameIntervalP - 1);
1088 
1089  return 0;
1090 }
1091 
1092 static av_cold int nvenc_setup_rate_control(AVCodecContext *avctx)
1093 {
1094  NvencContext *ctx = avctx->priv_data;
1095 
1096  if (avctx->global_quality > 0)
1097  av_log(avctx, AV_LOG_WARNING, "Using global_quality with nvenc is deprecated. Use qp instead.\n");
1098 
1099  if (ctx->cqp < 0 && avctx->global_quality > 0)
1100  ctx->cqp = avctx->global_quality;
1101 
1102  if (avctx->bit_rate > 0) {
1103  ctx->encode_config.rcParams.averageBitRate = avctx->bit_rate;
1104  } else if (ctx->encode_config.rcParams.averageBitRate > 0) {
1105  ctx->encode_config.rcParams.maxBitRate = ctx->encode_config.rcParams.averageBitRate;
1106  }
1107 
1108  if (avctx->rc_max_rate > 0)
1109  ctx->encode_config.rcParams.maxBitRate = avctx->rc_max_rate;
1110 
1111 #ifdef NVENC_HAVE_MULTIPASS
1112  ctx->encode_config.rcParams.multiPass = ctx->multipass;
1113 
1114  if (ctx->flags & NVENC_ONE_PASS)
1115  ctx->encode_config.rcParams.multiPass = NV_ENC_MULTI_PASS_DISABLED;
1116  if (ctx->flags & NVENC_TWO_PASSES || ctx->twopass > 0)
1117  ctx->encode_config.rcParams.multiPass = NV_ENC_TWO_PASS_FULL_RESOLUTION;
1118 
1119  if (ctx->rc < 0) {
1120  if (ctx->cbr) {
1121  ctx->rc = NV_ENC_PARAMS_RC_CBR;
1122  } else if (ctx->cqp >= 0) {
1123  ctx->rc = NV_ENC_PARAMS_RC_CONSTQP;
1124  } else if (ctx->quality >= 0.0f) {
1125  ctx->rc = NV_ENC_PARAMS_RC_VBR;
1126  }
1127  }
1128 #else
1129  if (ctx->rc < 0) {
1130  if (ctx->flags & NVENC_ONE_PASS)
1131  ctx->twopass = 0;
1132  if (ctx->flags & NVENC_TWO_PASSES)
1133  ctx->twopass = 1;
1134 
1135  if (ctx->twopass < 0)
1136  ctx->twopass = (ctx->flags & NVENC_LOWLATENCY) != 0;
1137 
1138  if (ctx->cbr) {
1139  if (ctx->twopass) {
1140  ctx->rc = NV_ENC_PARAMS_RC_CBR_LOWDELAY_HQ;
1141  } else {
1142  ctx->rc = NV_ENC_PARAMS_RC_CBR;
1143  }
1144  } else if (ctx->cqp >= 0) {
1145  ctx->rc = NV_ENC_PARAMS_RC_CONSTQP;
1146  } else if (ctx->twopass) {
1147  ctx->rc = NV_ENC_PARAMS_RC_VBR_HQ;
1148  } else if ((avctx->qmin >= 0 && avctx->qmax >= 0) ||
1149  (ctx->qmin >= 0 && ctx->qmax >= 0)) {
1150  ctx->rc = NV_ENC_PARAMS_RC_VBR_MINQP;
1151  }
1152  }
1153 #endif
1154 
1155  if (ctx->rc >= 0 && ctx->rc & RC_MODE_DEPRECATED) {
1156  av_log(avctx, AV_LOG_WARNING, "Specified rc mode is deprecated.\n");
1157  av_log(avctx, AV_LOG_WARNING, "Use -rc constqp/cbr/vbr, -tune and -multipass instead.\n");
1158 
1159  ctx->rc &= ~RC_MODE_DEPRECATED;
1160  }
1161 
1162 #ifdef NVENC_HAVE_QP_CHROMA_OFFSETS
1163  ctx->encode_config.rcParams.cbQPIndexOffset = ctx->qp_cb_offset;
1164  ctx->encode_config.rcParams.crQPIndexOffset = ctx->qp_cr_offset;
1165 
1166  if (avctx->codec->id == AV_CODEC_ID_AV1 &&
1167  ctx->qp_cr_offset != ctx->qp_cb_offset)
1168  av_log(avctx, AV_LOG_WARNING,
1169  "av1_nvenc: qp_cr_offset is currently ignored by the NVENC driver "
1170  "(deltaQ_v_ac is forced equal to deltaQ_u_ac); only qp_cb_offset "
1171  "takes effect.\n");
1172 #else
1173  if (ctx->qp_cb_offset || ctx->qp_cr_offset)
1174  av_log(avctx, AV_LOG_WARNING, "Failed setting QP CB/CR offsets, SDK 11.1 or greater required at compile time.\n");
1175 #endif
1176 
1177 #ifdef NVENC_HAVE_LDKFS
1178  if (ctx->ldkfs)
1179  ctx->encode_config.rcParams.lowDelayKeyFrameScale = ctx->ldkfs;
1180 #endif
1181 
1182  if (ctx->flags & NVENC_LOSSLESS) {
1183  set_lossless(avctx);
1184  } else if (ctx->rc >= 0) {
1185  nvenc_override_rate_control(avctx);
1186  } else {
1187  ctx->encode_config.rcParams.rateControlMode = NV_ENC_PARAMS_RC_VBR;
1188  set_vbr(avctx);
1189  }
1190 
1191  if (avctx->rc_buffer_size > 0) {
1192  ctx->encode_config.rcParams.vbvBufferSize = avctx->rc_buffer_size;
1193  } else if (ctx->encode_config.rcParams.averageBitRate > 0) {
1194  avctx->rc_buffer_size = ctx->encode_config.rcParams.vbvBufferSize = 2 * ctx->encode_config.rcParams.averageBitRate;
1195  }
1196 
1197  if (ctx->aq) {
1198  ctx->encode_config.rcParams.enableAQ = 1;
1199  ctx->encode_config.rcParams.aqStrength = ctx->aq_strength;
1200  av_log(avctx, AV_LOG_VERBOSE, "AQ enabled.\n");
1201  }
1202 
1203  if (ctx->temporal_aq) {
1204  ctx->encode_config.rcParams.enableTemporalAQ = 1;
1205  av_log(avctx, AV_LOG_VERBOSE, "Temporal AQ enabled.\n");
1206  }
1207 
1208  if (ctx->rc_lookahead > 0) {
1209  int lkd_bound = FFMIN(ctx->nb_surfaces, ctx->async_depth) -
1210  ctx->encode_config.frameIntervalP - 4;
1211 
1212  if (lkd_bound < 0) {
1213  ctx->encode_config.rcParams.enableLookahead = 0;
1214  av_log(avctx, AV_LOG_WARNING,
1215  "Lookahead not enabled. Increase buffer delay (-delay).\n");
1216  } else {
1217  ctx->encode_config.rcParams.enableLookahead = 1;
1218  ctx->encode_config.rcParams.lookaheadDepth = av_clip(ctx->rc_lookahead, 0, lkd_bound);
1219  ctx->encode_config.rcParams.disableIadapt = ctx->no_scenecut;
1220  ctx->encode_config.rcParams.disableBadapt = !ctx->b_adapt;
1221  av_log(avctx, AV_LOG_VERBOSE,
1222  "Lookahead enabled: depth %d, scenecut %s, B-adapt %s.\n",
1223  ctx->encode_config.rcParams.lookaheadDepth,
1224  ctx->encode_config.rcParams.disableIadapt ? "disabled" : "enabled",
1225  ctx->encode_config.rcParams.disableBadapt ? "disabled" : "enabled");
1226  if (ctx->encode_config.rcParams.lookaheadDepth < ctx->rc_lookahead)
1227  av_log(avctx, AV_LOG_WARNING, "Clipping lookahead depth to %d (from %d) due to lack of surfaces/delay",
1228  ctx->encode_config.rcParams.lookaheadDepth, ctx->rc_lookahead);
1229 
1230 #ifdef NVENC_HAVE_LOOKAHEAD_LEVEL
1231  if (ctx->lookahead_level >= 0) {
1232  switch (ctx->lookahead_level) {
1233  case NV_ENC_LOOKAHEAD_LEVEL_0:
1234  case NV_ENC_LOOKAHEAD_LEVEL_1:
1235  case NV_ENC_LOOKAHEAD_LEVEL_2:
1236  case NV_ENC_LOOKAHEAD_LEVEL_3:
1237  case NV_ENC_LOOKAHEAD_LEVEL_AUTOSELECT:
1238  break;
1239  default:
1240  av_log(avctx, AV_LOG_ERROR, "Invalid lookahead level.\n");
1241  return AVERROR(EINVAL);
1242  }
1243 
1244  ctx->encode_config.rcParams.lookaheadLevel = ctx->lookahead_level;
1245  }
1246 #endif
1247  }
1248  }
1249 
1250  if (ctx->strict_gop) {
1251  ctx->encode_config.rcParams.strictGOPTarget = 1;
1252  av_log(avctx, AV_LOG_VERBOSE, "Strict GOP target enabled.\n");
1253  }
1254 
1255  if (ctx->nonref_p)
1256  ctx->encode_config.rcParams.enableNonRefP = 1;
1257 
1258  if (ctx->zerolatency)
1259  ctx->encode_config.rcParams.zeroReorderDelay = 1;
1260 
1261  if (ctx->quality) {
1262  //convert from float to fixed point 8.8
1263  int tmp_quality = (int)(ctx->quality * 256.0f);
1264  ctx->encode_config.rcParams.targetQuality = (uint8_t)(tmp_quality >> 8);
1265  ctx->encode_config.rcParams.targetQualityLSB = (uint8_t)(tmp_quality & 0xff);
1266 
1267  av_log(avctx, AV_LOG_VERBOSE, "CQ(%d) mode enabled.\n", tmp_quality);
1268 
1269  // CQ mode shall discard avg bitrate/vbv buffer size and honor only max bitrate
1270  ctx->encode_config.rcParams.averageBitRate = avctx->bit_rate = 0;
1271  ctx->encode_config.rcParams.vbvBufferSize = avctx->rc_buffer_size = 0;
1272  ctx->encode_config.rcParams.maxBitRate = avctx->rc_max_rate;
1273  }
1274 
1275  return 0;
1276 }
1277 
1278 static av_cold int nvenc_setup_h264_config(AVCodecContext *avctx)
1279 {
1280  NvencContext *ctx = avctx->priv_data;
1281  NV_ENC_CONFIG *cc = &ctx->encode_config;
1282  NV_ENC_CONFIG_H264 *h264 = &cc->encodeCodecConfig.h264Config;
1283  NV_ENC_CONFIG_H264_VUI_PARAMETERS *vui = &h264->h264VUIParameters;
1284 
1285  const AVPixFmtDescriptor *pixdesc = av_pix_fmt_desc_get(ctx->data_pix_fmt);
1286 
1287  if ((pixdesc->flags & AV_PIX_FMT_FLAG_RGB) && !IS_GBRP(ctx->data_pix_fmt)) {
1288  vui->colourMatrix = to_nv_color_matrix(AVCOL_SPC_BT470BG);
1289  vui->colourPrimaries = to_nv_color_pri(avctx->color_primaries);
1290  vui->transferCharacteristics = to_nv_color_trc(avctx->color_trc);
1291  vui->videoFullRangeFlag = 0;
1292  } else {
1293  vui->colourMatrix = to_nv_color_matrix(IS_GBRP(ctx->data_pix_fmt) ? AVCOL_SPC_RGB : avctx->colorspace);
1294  vui->colourPrimaries = to_nv_color_pri(avctx->color_primaries);
1295  vui->transferCharacteristics = to_nv_color_trc(avctx->color_trc);
1296  vui->videoFullRangeFlag = (avctx->color_range == AVCOL_RANGE_JPEG
1297  || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ420P || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ422P || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ444P);
1298  }
1299 
1300  vui->colourDescriptionPresentFlag =
1301  (vui->colourMatrix != 2 || vui->colourPrimaries != 2 || vui->transferCharacteristics != 2);
1302 
1303  vui->videoSignalTypePresentFlag =
1304  (vui->colourDescriptionPresentFlag
1305  || vui->videoFormat != 5
1306  || vui->videoFullRangeFlag != 0);
1307 
1308  if (ctx->max_slice_size > 0) {
1309  h264->sliceMode = 1;
1310  h264->sliceModeData = ctx->max_slice_size;
1311  } else {
1312  h264->sliceMode = 3;
1313  h264->sliceModeData = avctx->slices > 0 ? avctx->slices : 1;
1314  }
1315 
1316  if (ctx->intra_refresh) {
1317  h264->enableIntraRefresh = 1;
1318  h264->intraRefreshPeriod = cc->gopLength;
1319  h264->intraRefreshCnt = cc->gopLength - 1;
1320  cc->gopLength = NVENC_INFINITE_GOPLENGTH;
1321  h264->outputRecoveryPointSEI = 1;
1322 #ifdef NVENC_HAVE_SINGLE_SLICE_INTRA_REFRESH
1323  h264->singleSliceIntraRefresh = ctx->single_slice_intra_refresh;
1324 #endif
1325  }
1326 
1327  if (ctx->constrained_encoding)
1328  h264->enableConstrainedEncoding = 1;
1329 
1330  h264->disableSPSPPS = (avctx->flags & AV_CODEC_FLAG_GLOBAL_HEADER) ? 1 : 0;
1331  h264->repeatSPSPPS = (avctx->flags & AV_CODEC_FLAG_GLOBAL_HEADER) ? 0 : 1;
1332  h264->outputAUD = ctx->aud;
1333 
1334  if (ctx->dpb_size >= 0) {
1335  /* 0 means "let the hardware decide" */
1336  h264->maxNumRefFrames = ctx->dpb_size;
1337  }
1338 
1339  h264->idrPeriod = cc->gopLength;
1340 
1341  if (IS_CBR(cc->rcParams.rateControlMode)) {
1342  /* Older SDKs use outputBufferingPeriodSEI to control filler data */
1343  h264->outputBufferingPeriodSEI = ctx->cbr_padding;
1344 
1345 #ifdef NVENC_HAVE_FILLER_DATA
1346  h264->enableFillerDataInsertion = ctx->cbr_padding;
1347 #endif
1348  }
1349 
1350  h264->outputPictureTimingSEI = 1;
1351 
1352 #ifndef NVENC_NO_DEPRECATED_RC
1353  if (cc->rcParams.rateControlMode == NV_ENC_PARAMS_RC_CBR_LOWDELAY_HQ ||
1354  cc->rcParams.rateControlMode == NV_ENC_PARAMS_RC_CBR_HQ ||
1355  cc->rcParams.rateControlMode == NV_ENC_PARAMS_RC_VBR_HQ) {
1356  h264->adaptiveTransformMode = NV_ENC_H264_ADAPTIVE_TRANSFORM_ENABLE;
1357  h264->fmoMode = NV_ENC_H264_FMO_DISABLE;
1358  }
1359 #endif
1360 
1361  if (ctx->flags & NVENC_LOSSLESS) {
1362  h264->qpPrimeYZeroTransformBypassFlag = 1;
1363  } else {
1364  switch(ctx->profile) {
1365  case NV_ENC_H264_PROFILE_BASELINE:
1366  cc->profileGUID = NV_ENC_H264_PROFILE_BASELINE_GUID;
1367  avctx->profile = AV_PROFILE_H264_BASELINE;
1368  if (cc->frameIntervalP > 1) {
1369  av_log(avctx, AV_LOG_WARNING,
1370  "B-frames are not supported by H.264 Baseline profile, disabling.\n");
1371  cc->frameIntervalP = 1;
1372  }
1373  break;
1374  case NV_ENC_H264_PROFILE_MAIN:
1375  cc->profileGUID = NV_ENC_H264_PROFILE_MAIN_GUID;
1376  avctx->profile = AV_PROFILE_H264_MAIN;
1377  break;
1378  case NV_ENC_H264_PROFILE_HIGH:
1379  cc->profileGUID = NV_ENC_H264_PROFILE_HIGH_GUID;
1380  avctx->profile = AV_PROFILE_H264_HIGH;
1381  break;
1382 #ifdef NVENC_HAVE_H264_10BIT_SUPPORT
1383  case NV_ENC_H264_PROFILE_HIGH_10:
1384  cc->profileGUID = NV_ENC_H264_PROFILE_HIGH_10_GUID;
1385  avctx->profile = AV_PROFILE_H264_HIGH_10;
1386  break;
1387 #endif
1388 #ifdef NVENC_HAVE_422_SUPPORT
1389  case NV_ENC_H264_PROFILE_HIGH_422:
1390  cc->profileGUID = NV_ENC_H264_PROFILE_HIGH_422_GUID;
1391  avctx->profile = AV_PROFILE_H264_HIGH_422;
1392  break;
1393 #endif
1394  case NV_ENC_H264_PROFILE_HIGH_444P:
1395  cc->profileGUID = NV_ENC_H264_PROFILE_HIGH_444_GUID;
1396  avctx->profile = AV_PROFILE_H264_HIGH_444_PREDICTIVE;
1397  break;
1398  }
1399  }
1400 
1401 #ifdef NVENC_HAVE_H264_10BIT_SUPPORT
1402  // force setting profile as high10 if input is 10 bit or if it should be encoded as 10 bit
1403  if (IS_10BIT(ctx->data_pix_fmt) || ctx->highbitdepth) {
1404  cc->profileGUID = NV_ENC_H264_PROFILE_HIGH_10_GUID;
1405  avctx->profile = AV_PROFILE_H264_HIGH_10;
1406  }
1407 #endif
1408 
1409  // force setting profile as high444p if input is AV_PIX_FMT_YUV444P
1410  if (IS_YUV444(ctx->data_pix_fmt)) {
1411  cc->profileGUID = NV_ENC_H264_PROFILE_HIGH_444_GUID;
1412  avctx->profile = AV_PROFILE_H264_HIGH_444_PREDICTIVE;
1413  }
1414 
1415 #ifdef NVENC_HAVE_422_SUPPORT
1416  // force setting profile as high422p if input is AV_PIX_FMT_YUV422P
1417  if (IS_YUV422(ctx->data_pix_fmt)) {
1418  cc->profileGUID = NV_ENC_H264_PROFILE_HIGH_422_GUID;
1419  avctx->profile = AV_PROFILE_H264_HIGH_422;
1420  }
1421 #endif
1422 
1423  vui->bitstreamRestrictionFlag = cc->gopLength != 1 || avctx->profile < AV_PROFILE_H264_HIGH;
1424 
1425  h264->chromaFormatIDC = IS_YUV444(ctx->data_pix_fmt) ? 3 : IS_YUV422(ctx->data_pix_fmt) ? 2 : 1;
1426 
1427  h264->level = ctx->level;
1428 
1429 #ifdef NVENC_HAVE_NEW_BIT_DEPTH_API
1430  h264->inputBitDepth = IS_10BIT(ctx->data_pix_fmt) ? NV_ENC_BIT_DEPTH_10 : NV_ENC_BIT_DEPTH_8;
1431  h264->outputBitDepth = (IS_10BIT(ctx->data_pix_fmt) || ctx->highbitdepth) ? NV_ENC_BIT_DEPTH_10 : NV_ENC_BIT_DEPTH_8;
1432 #endif
1433 
1434  if (ctx->coder >= 0)
1435  h264->entropyCodingMode = ctx->coder;
1436 
1437 #ifdef NVENC_HAVE_BFRAME_REF_MODE
1438  if (ctx->b_ref_mode >= 0)
1439  h264->useBFramesAsRef = ctx->b_ref_mode;
1440 #endif
1441 
1442 #ifdef NVENC_HAVE_MULTIPLE_REF_FRAMES
1443  h264->numRefL0 = avctx->refs;
1444  h264->numRefL1 = avctx->refs;
1445 #endif
1446 
1447 #ifdef NVENC_HAVE_H264_AND_AV1_TEMPORAL_FILTER
1448  if (ctx->tf_level >= 0) {
1449  h264->tfLevel = ctx->tf_level;
1450 
1451  switch (ctx->tf_level)
1452  {
1453  case NV_ENC_TEMPORAL_FILTER_LEVEL_0:
1454  case NV_ENC_TEMPORAL_FILTER_LEVEL_4:
1455  break;
1456  default:
1457  av_log(avctx, AV_LOG_ERROR, "Invalid temporal filtering level.\n");
1458  return AVERROR(EINVAL);
1459  }
1460 
1461  if (ctx->encode_config.frameIntervalP < 5)
1462  av_log(avctx, AV_LOG_WARNING, "Temporal filtering needs at least 4 B-Frames (-bf 4).\n");
1463  }
1464 #endif
1465 
1466 #ifdef NVENC_HAVE_TIME_CODE
1467  if (ctx->s12m_tc)
1468  h264->enableTimeCode = 1;
1469 #endif
1470 
1471  return 0;
1472 }
1473 
1474 static av_cold int nvenc_setup_hevc_config(AVCodecContext *avctx)
1475 {
1476  NvencContext *ctx = avctx->priv_data;
1477  NV_ENC_CONFIG *cc = &ctx->encode_config;
1478  NV_ENC_CONFIG_HEVC *hevc = &cc->encodeCodecConfig.hevcConfig;
1479  NV_ENC_CONFIG_HEVC_VUI_PARAMETERS *vui = &hevc->hevcVUIParameters;
1480 
1481  const AVPixFmtDescriptor *pixdesc = av_pix_fmt_desc_get(ctx->data_pix_fmt);
1482 
1483  if ((pixdesc->flags & AV_PIX_FMT_FLAG_RGB) && !IS_GBRP(ctx->data_pix_fmt)) {
1484  vui->colourMatrix = to_nv_color_matrix(AVCOL_SPC_BT470BG);
1485  vui->colourPrimaries = to_nv_color_pri(avctx->color_primaries);
1486  vui->transferCharacteristics = to_nv_color_trc(avctx->color_trc);
1487  vui->videoFullRangeFlag = 0;
1488  } else {
1489  vui->colourMatrix = to_nv_color_matrix(IS_GBRP(ctx->data_pix_fmt) ? AVCOL_SPC_RGB : avctx->colorspace);
1490  vui->colourPrimaries = to_nv_color_pri(avctx->color_primaries);
1491  vui->transferCharacteristics = to_nv_color_trc(avctx->color_trc);
1492  vui->videoFullRangeFlag = (avctx->color_range == AVCOL_RANGE_JPEG
1493  || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ420P || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ422P || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ444P);
1494  }
1495 
1496  vui->colourDescriptionPresentFlag =
1497  (vui->colourMatrix != 2 || vui->colourPrimaries != 2 || vui->transferCharacteristics != 2);
1498 
1499  vui->videoSignalTypePresentFlag =
1500  (vui->colourDescriptionPresentFlag
1501  || vui->videoFormat != 5
1502  || vui->videoFullRangeFlag != 0);
1503 
1504  if (ctx->max_slice_size > 0) {
1505  hevc->sliceMode = 1;
1506  hevc->sliceModeData = ctx->max_slice_size;
1507  } else {
1508  hevc->sliceMode = 3;
1509  hevc->sliceModeData = avctx->slices > 0 ? avctx->slices : 1;
1510  }
1511 
1512  if (ctx->intra_refresh) {
1513  hevc->enableIntraRefresh = 1;
1514  hevc->intraRefreshPeriod = cc->gopLength;
1515  hevc->intraRefreshCnt = cc->gopLength - 1;
1516  cc->gopLength = NVENC_INFINITE_GOPLENGTH;
1517 #ifdef NVENC_HAVE_HEVC_OUTPUT_RECOVERY_POINT_SEI
1518  hevc->outputRecoveryPointSEI = 1;
1519 #endif
1520 #ifdef NVENC_HAVE_SINGLE_SLICE_INTRA_REFRESH
1521  hevc->singleSliceIntraRefresh = ctx->single_slice_intra_refresh;
1522 #endif
1523  }
1524 
1525 #ifdef NVENC_HAVE_HEVC_AND_AV1_MASTERING_METADATA
1526  ctx->mdm = hevc->outputMasteringDisplay = !!av_frame_side_data_get(avctx->decoded_side_data,
1527  avctx->nb_decoded_side_data,
1528  AV_FRAME_DATA_MASTERING_DISPLAY_METADATA);
1529  ctx->cll = hevc->outputMaxCll = !!av_frame_side_data_get(avctx->decoded_side_data,
1530  avctx->nb_decoded_side_data,
1531  AV_FRAME_DATA_CONTENT_LIGHT_LEVEL);
1532 #endif
1533 
1534 #ifdef NVENC_HAVE_HEVC_CONSTRAINED_ENCODING
1535  if (ctx->constrained_encoding)
1536  hevc->enableConstrainedEncoding = 1;
1537 #endif
1538 
1539  hevc->disableSPSPPS = (avctx->flags & AV_CODEC_FLAG_GLOBAL_HEADER) ? 1 : 0;
1540  hevc->repeatSPSPPS = (avctx->flags & AV_CODEC_FLAG_GLOBAL_HEADER) ? 0 : 1;
1541  hevc->outputAUD = ctx->aud;
1542 
1543  if (ctx->dpb_size >= 0) {
1544  /* 0 means "let the hardware decide" */
1545  hevc->maxNumRefFramesInDPB = ctx->dpb_size;
1546  }
1547 
1548  hevc->idrPeriod = cc->gopLength;
1549 
1550  if (IS_CBR(cc->rcParams.rateControlMode)) {
1551  /* Older SDKs use outputBufferingPeriodSEI to control filler data */
1552  hevc->outputBufferingPeriodSEI = ctx->cbr_padding;
1553 
1554 #ifdef NVENC_HAVE_FILLER_DATA
1555  hevc->enableFillerDataInsertion = ctx->cbr_padding;
1556 #endif
1557  }
1558 
1559  hevc->outputPictureTimingSEI = 1;
1560 
1561 #ifdef NVENC_HAVE_MVHEVC
1562  if (ctx->multiview_supported && (ctx->profile == NV_ENC_HEVC_PROFILE_MAIN || ctx->profile == NV_ENC_HEVC_PROFILE_MULTIVIEW_MAIN)) {
1563  const AVFrameSideData *sd_stereo3d = av_frame_side_data_get(avctx->decoded_side_data, avctx->nb_decoded_side_data, AV_FRAME_DATA_STEREO3D);
1564  const AVFrameSideData *sd_tdrdi = av_frame_side_data_get(avctx->decoded_side_data, avctx->nb_decoded_side_data, AV_FRAME_DATA_3D_REFERENCE_DISPLAYS);
1565  const AVStereo3D *stereo3d = sd_stereo3d ? (const AVStereo3D*)sd_stereo3d->data : NULL;
1566 
1567  if (sd_tdrdi && stereo3d && stereo3d->type == AV_STEREO3D_FRAMESEQUENCE)
1568  ctx->profile = NV_ENC_HEVC_PROFILE_MULTIVIEW_MAIN;
1569 
1570  if (ctx->profile == NV_ENC_HEVC_PROFILE_MULTIVIEW_MAIN && stereo3d &&
1571  stereo3d->type != AV_STEREO3D_2D &&
1572  stereo3d->type != AV_STEREO3D_UNSPEC &&
1573  stereo3d->type != AV_STEREO3D_FRAMESEQUENCE)
1574  {
1575  av_log(avctx, AV_LOG_WARNING, "Unsupported multiview input, disabling multiview encoding.\n");
1576  ctx->profile = NV_ENC_HEVC_PROFILE_MAIN;
1577  }
1578  }
1579 #endif
1580 
1581  switch (ctx->profile) {
1582  case NV_ENC_HEVC_PROFILE_MAIN:
1583  cc->profileGUID = NV_ENC_HEVC_PROFILE_MAIN_GUID;
1584  avctx->profile = AV_PROFILE_HEVC_MAIN;
1585  break;
1586  case NV_ENC_HEVC_PROFILE_MAIN_10:
1587  cc->profileGUID = NV_ENC_HEVC_PROFILE_MAIN10_GUID;
1588  avctx->profile = AV_PROFILE_HEVC_MAIN_10;
1589  break;
1590  case NV_ENC_HEVC_PROFILE_REXT:
1591  cc->profileGUID = NV_ENC_HEVC_PROFILE_FREXT_GUID;
1592  avctx->profile = AV_PROFILE_HEVC_REXT;
1593  break;
1594 #ifdef NVENC_HAVE_MVHEVC
1595  case NV_ENC_HEVC_PROFILE_MULTIVIEW_MAIN:
1596  cc->profileGUID = NV_ENC_HEVC_PROFILE_MAIN_GUID;
1597  avctx->profile = AV_PROFILE_HEVC_MULTIVIEW_MAIN;
1598  ctx->multiview = 1;
1599 
1600  hevc->enableMVHEVC = 1;
1601  hevc->outputHevc3DReferenceDisplayInfo = 1;
1602 
1603  av_log(avctx, AV_LOG_VERBOSE, "Enabling MV HEVC encoding.\n");
1604  break;
1605 #endif
1606  }
1607 
1608  // force setting profile as main10 if input is 10 bit or if it should be encoded as 10 bit
1609  if (IS_10BIT(ctx->data_pix_fmt) || ctx->highbitdepth) {
1610  cc->profileGUID = NV_ENC_HEVC_PROFILE_MAIN10_GUID;
1611  avctx->profile = AV_PROFILE_HEVC_MAIN_10;
1612  }
1613 
1614  // force setting profile as rext if input is yuv444 or yuv422
1615  if (IS_YUV444(ctx->data_pix_fmt) || IS_YUV422(ctx->data_pix_fmt)) {
1616  cc->profileGUID = NV_ENC_HEVC_PROFILE_FREXT_GUID;
1617  avctx->profile = AV_PROFILE_HEVC_REXT;
1618  }
1619 
1620 #ifdef NVENC_HAVE_MVHEVC
1621  if (ctx->multiview && avctx->profile != AV_PROFILE_HEVC_MULTIVIEW_MAIN) {
1622  av_log(avctx, AV_LOG_ERROR, "Multiview encoding only works for Main profile content.\n");
1623  return AVERROR(EINVAL);
1624  }
1625 #endif
1626 
1627  hevc->chromaFormatIDC = IS_YUV444(ctx->data_pix_fmt) ? 3 : IS_YUV422(ctx->data_pix_fmt) ? 2 : 1;
1628 
1629 #ifdef NVENC_HAVE_NEW_BIT_DEPTH_API
1630  hevc->inputBitDepth = IS_10BIT(ctx->data_pix_fmt) ? NV_ENC_BIT_DEPTH_10 : NV_ENC_BIT_DEPTH_8;
1631  hevc->outputBitDepth = (IS_10BIT(ctx->data_pix_fmt) || ctx->highbitdepth) ? NV_ENC_BIT_DEPTH_10 : NV_ENC_BIT_DEPTH_8;
1632 #else
1633  hevc->pixelBitDepthMinus8 = IS_10BIT(ctx->data_pix_fmt) ? 2 : 0;
1634 #endif
1635 
1636  hevc->level = ctx->level;
1637 
1638  hevc->tier = ctx->tier;
1639 
1640 #ifdef NVENC_HAVE_HEVC_BFRAME_REF_MODE
1641  if (ctx->b_ref_mode >= 0)
1642  hevc->useBFramesAsRef = ctx->b_ref_mode;
1643 #endif
1644 
1645 #ifdef NVENC_HAVE_MULTIPLE_REF_FRAMES
1646  hevc->numRefL0 = avctx->refs;
1647  hevc->numRefL1 = avctx->refs;
1648 #endif
1649 
1650 #ifdef NVENC_HAVE_TEMPORAL_FILTER
1651  if (ctx->tf_level >= 0) {
1652  hevc->tfLevel = ctx->tf_level;
1653 
1654  switch (ctx->tf_level)
1655  {
1656  case NV_ENC_TEMPORAL_FILTER_LEVEL_0:
1657  case NV_ENC_TEMPORAL_FILTER_LEVEL_4:
1658  break;
1659  default:
1660  av_log(avctx, AV_LOG_ERROR, "Invalid temporal filtering level.\n");
1661  return AVERROR(EINVAL);
1662  }
1663 
1664  if (ctx->encode_config.frameIntervalP < 5)
1665  av_log(avctx, AV_LOG_WARNING, "Temporal filtering needs at least 4 B-Frames (-bf 4).\n");
1666  }
1667 #endif
1668 
1669  return 0;
1670 }
1671 
1672 #if CONFIG_AV1_NVENC_ENCODER
1673 static av_cold int nvenc_setup_av1_config(AVCodecContext *avctx)
1674 {
1675  NvencContext *ctx = avctx->priv_data;
1676  NV_ENC_CONFIG *cc = &ctx->encode_config;
1677  NV_ENC_CONFIG_AV1 *av1 = &cc->encodeCodecConfig.av1Config;
1678 
1679  const AVPixFmtDescriptor *pixdesc = av_pix_fmt_desc_get(ctx->data_pix_fmt);
1680 
1681  if ((pixdesc->flags & AV_PIX_FMT_FLAG_RGB) && !IS_GBRP(ctx->data_pix_fmt)) {
1682  av1->matrixCoefficients = to_nv_color_matrix(AVCOL_SPC_BT470BG);
1683  av1->colorPrimaries = to_nv_color_pri(avctx->color_primaries);
1684  av1->transferCharacteristics = to_nv_color_trc(avctx->color_trc);
1685  av1->colorRange = 0;
1686  } else {
1687  av1->matrixCoefficients = to_nv_color_matrix(IS_GBRP(ctx->data_pix_fmt) ? AVCOL_SPC_RGB : avctx->colorspace);
1688  av1->colorPrimaries = to_nv_color_pri(avctx->color_primaries);
1689  av1->transferCharacteristics = to_nv_color_trc(avctx->color_trc);
1690  av1->colorRange = (avctx->color_range == AVCOL_RANGE_JPEG
1691  || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ420P || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ422P || ctx->data_pix_fmt == AV_PIX_FMT_YUVJ444P);
1692  }
1693 
1694  if (IS_YUV444(ctx->data_pix_fmt)) {
1695  av_log(avctx, AV_LOG_ERROR, "AV1 High Profile not supported, required for 4:4:4 encoding\n");
1696  return AVERROR(ENOTSUP);
1697  } else {
1698  cc->profileGUID = NV_ENC_AV1_PROFILE_MAIN_GUID;
1699  avctx->profile = AV_PROFILE_AV1_MAIN;
1700  }
1701 
1702  if (ctx->dpb_size >= 0) {
1703  /* 0 means "let the hardware decide" */
1704  av1->maxNumRefFramesInDPB = ctx->dpb_size;
1705  }
1706 
1707  if (ctx->intra_refresh) {
1708  av1->enableIntraRefresh = 1;
1709  av1->intraRefreshPeriod = cc->gopLength;
1710  av1->intraRefreshCnt = cc->gopLength - 1;
1711  cc->gopLength = NVENC_INFINITE_GOPLENGTH;
1712  }
1713 
1714  av1->idrPeriod = cc->gopLength;
1715 
1716  if (IS_CBR(cc->rcParams.rateControlMode)) {
1717  av1->enableBitstreamPadding = ctx->cbr_padding;
1718  }
1719 
1720  if (ctx->tile_cols >= 0)
1721  av1->numTileColumns = ctx->tile_cols;
1722  if (ctx->tile_rows >= 0)
1723  av1->numTileRows = ctx->tile_rows;
1724 
1725  av1->outputAnnexBFormat = 0;
1726 
1727  av1->level = ctx->level;
1728  av1->tier = ctx->tier;
1729 
1730  av1->enableTimingInfo = ctx->timing_info;
1731 
1732  /* mp4 encapsulation requires sequence headers to be present on all keyframes for AV1 */
1733  av1->disableSeqHdr = 0;
1734  av1->repeatSeqHdr = 1;
1735 
1736  av1->chromaFormatIDC = IS_YUV444(ctx->data_pix_fmt) ? 3 : 1;
1737 
1738 #ifdef NVENC_HAVE_NEW_BIT_DEPTH_API
1739  av1->inputBitDepth = IS_10BIT(ctx->data_pix_fmt) ? NV_ENC_BIT_DEPTH_10 : NV_ENC_BIT_DEPTH_8;
1740  av1->outputBitDepth = (IS_10BIT(ctx->data_pix_fmt) || ctx->highbitdepth) ? NV_ENC_BIT_DEPTH_10 : NV_ENC_BIT_DEPTH_8;
1741 #else
1742  av1->inputPixelBitDepthMinus8 = IS_10BIT(ctx->data_pix_fmt) ? 2 : 0;
1743  av1->pixelBitDepthMinus8 = (IS_10BIT(ctx->data_pix_fmt) || ctx->highbitdepth) ? 2 : 0;
1744 #endif
1745 
1746 #ifdef NVENC_HAVE_HEVC_AND_AV1_MASTERING_METADATA
1747  ctx->mdm = av1->outputMasteringDisplay = !!av_frame_side_data_get(avctx->decoded_side_data,
1748  avctx->nb_decoded_side_data,
1749  AV_FRAME_DATA_MASTERING_DISPLAY_METADATA);
1750  ctx->cll = av1->outputMaxCll = !!av_frame_side_data_get(avctx->decoded_side_data,
1751  avctx->nb_decoded_side_data,
1752  AV_FRAME_DATA_CONTENT_LIGHT_LEVEL);
1753 #endif
1754 
1755  if (ctx->b_ref_mode >= 0)
1756  av1->useBFramesAsRef = ctx->b_ref_mode;
1757 
1758  av1->numFwdRefs = avctx->refs;
1759  av1->numBwdRefs = avctx->refs;
1760 
1761 #ifdef NVENC_HAVE_H264_AND_AV1_TEMPORAL_FILTER
1762  if (ctx->tf_level >= 0) {
1763  av1->tfLevel = ctx->tf_level;
1764 
1765  switch (ctx->tf_level)
1766  {
1767  case NV_ENC_TEMPORAL_FILTER_LEVEL_0:
1768  case NV_ENC_TEMPORAL_FILTER_LEVEL_4:
1769  break;
1770  default:
1771  av_log(avctx, AV_LOG_ERROR, "Invalid temporal filtering level.\n");
1772  return AVERROR(EINVAL);
1773  }
1774 
1775  if (ctx->encode_config.frameIntervalP < 5)
1776  av_log(avctx, AV_LOG_WARNING, "Temporal filtering needs at least 4 B-Frames (-bf 4).\n");
1777  }
1778 #endif
1779 
1780  return 0;
1781 }
1782 #endif
1783 
1784 static av_cold int nvenc_setup_codec_config(AVCodecContext *avctx)
1785 {
1786  switch (avctx->codec->id) {
1787  case AV_CODEC_ID_H264:
1788  return nvenc_setup_h264_config(avctx);
1789  case AV_CODEC_ID_HEVC:
1790  return nvenc_setup_hevc_config(avctx);
1791 #if CONFIG_AV1_NVENC_ENCODER
1792  case AV_CODEC_ID_AV1:
1793  return nvenc_setup_av1_config(avctx);
1794 #endif
1795  /* Earlier switch/case will return if unknown codec is passed. */
1796  }
1797 
1798  return 0;
1799 }
1800 
1801 static void compute_dar(AVCodecContext *avctx, int *dw, int *dh) {
1802  int sw, sh;
1803 
1804  sw = avctx->width;
1805  sh = avctx->height;
1806 
1807 #if CONFIG_AV1_NVENC_ENCODER
1808  if (avctx->codec->id == AV_CODEC_ID_AV1) {
1809  /* For AV1 we actually need to calculate the render width/height, not the dar */
1810  if (avctx->sample_aspect_ratio.num > 0 && avctx->sample_aspect_ratio.den > 0
1811  && avctx->sample_aspect_ratio.num != avctx->sample_aspect_ratio.den)
1812  {
1813  if (avctx->sample_aspect_ratio.num > avctx->sample_aspect_ratio.den) {
1814  sw = av_rescale(sw, avctx->sample_aspect_ratio.num, avctx->sample_aspect_ratio.den);
1815  } else {
1816  sh = av_rescale(sh, avctx->sample_aspect_ratio.den, avctx->sample_aspect_ratio.num);
1817  }
1818  }
1819 
1820  *dw = sw;
1821  *dh = sh;
1822  return;
1823  }
1824 #endif
1825 
1826  if (avctx->sample_aspect_ratio.num > 0 && avctx->sample_aspect_ratio.den > 0) {
1827  sw *= avctx->sample_aspect_ratio.num;
1828  sh *= avctx->sample_aspect_ratio.den;
1829  }
1830 
1831  av_reduce(dw, dh, sw, sh, 1024 * 1024);
1832 }
1833 
1834 static av_cold int nvenc_setup_encoder(AVCodecContext *avctx)
1835 {
1836  NvencContext *ctx = avctx->priv_data;
1837  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
1838  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
1839 
1840  NV_ENC_PRESET_CONFIG preset_config = { 0 };
1841  NVENCSTATUS nv_status = NV_ENC_SUCCESS;
1842  AVCPBProperties *cpb_props;
1843  int res = 0;
1844  int dw, dh;
1845 
1846  ctx->encode_config.version = NV_ENC_CONFIG_VER;
1847  ctx->init_encode_params.version = NV_ENC_INITIALIZE_PARAMS_VER;
1848 
1849  ctx->init_encode_params.encodeHeight = avctx->height;
1850  ctx->init_encode_params.encodeWidth = avctx->width;
1851 
1852  ctx->init_encode_params.encodeConfig = &ctx->encode_config;
1853 
1854  preset_config.version = NV_ENC_PRESET_CONFIG_VER;
1855  preset_config.presetCfg.version = NV_ENC_CONFIG_VER;
1856 
1857 #ifdef NVENC_HAVE_NEW_PRESETS
1858  ctx->init_encode_params.tuningInfo = ctx->tuning_info;
1859 
1860  if (ctx->flags & NVENC_LOSSLESS)
1861  ctx->init_encode_params.tuningInfo = NV_ENC_TUNING_INFO_LOSSLESS;
1862  else if (ctx->flags & NVENC_LOWLATENCY)
1863  ctx->init_encode_params.tuningInfo = NV_ENC_TUNING_INFO_LOW_LATENCY;
1864 
1865  nv_status = p_nvenc->nvEncGetEncodePresetConfigEx(ctx->nvencoder,
1866  ctx->init_encode_params.encodeGUID,
1867  ctx->init_encode_params.presetGUID,
1868  ctx->init_encode_params.tuningInfo,
1869  &preset_config);
1870 #else
1871  nv_status = p_nvenc->nvEncGetEncodePresetConfig(ctx->nvencoder,
1872  ctx->init_encode_params.encodeGUID,
1873  ctx->init_encode_params.presetGUID,
1874  &preset_config);
1875 #endif
1876  if (nv_status != NV_ENC_SUCCESS)
1877  return nvenc_print_error(avctx, nv_status, "Cannot get the preset configuration");
1878 
1879  memcpy(&ctx->encode_config, &preset_config.presetCfg, sizeof(ctx->encode_config));
1880 
1881  ctx->encode_config.version = NV_ENC_CONFIG_VER;
1882 
1883  compute_dar(avctx, &dw, &dh);
1884  ctx->init_encode_params.darHeight = dh;
1885  ctx->init_encode_params.darWidth = dw;
1886 
1887  if (avctx->framerate.num > 0 && avctx->framerate.den > 0) {
1888  ctx->init_encode_params.frameRateNum = avctx->framerate.num;
1889  ctx->init_encode_params.frameRateDen = avctx->framerate.den;
1890  } else {
1891  ctx->init_encode_params.frameRateNum = avctx->time_base.den;
1892  ctx->init_encode_params.frameRateDen = avctx->time_base.num;
1893  }
1894 
1895 #ifdef NVENC_HAVE_UNIDIR_B
1896  ctx->init_encode_params.enableUniDirectionalB = ctx->unidir_b;
1897 #endif
1898 
1899  ctx->init_encode_params.enableEncodeAsync = 0;
1900  ctx->init_encode_params.enablePTD = 1;
1901 
1902 #ifdef NVENC_HAVE_NEW_PRESETS
1903  /* If lookahead isn't set from CLI, use value from preset.
1904  * P6 & P7 presets may enable lookahead for better quality.
1905  * */
1906  if (ctx->rc_lookahead == 0 && ctx->encode_config.rcParams.enableLookahead)
1907  ctx->rc_lookahead = ctx->encode_config.rcParams.lookaheadDepth;
1908 #endif
1909 
1910  if (ctx->weighted_pred == 1)
1911  ctx->init_encode_params.enableWeightedPrediction = 1;
1912 
1913 #ifdef NVENC_HAVE_SPLIT_FRAME_ENCODING
1914  ctx->init_encode_params.splitEncodeMode = ctx->split_encode_mode;
1915 
1916  if (ctx->split_encode_mode != NV_ENC_SPLIT_DISABLE_MODE) {
1917  if (avctx->codec->id == AV_CODEC_ID_HEVC && ctx->weighted_pred == 1)
1918  av_log(avctx, AV_LOG_WARNING, "Split encoding not supported with weighted prediction enabled.\n");
1919  }
1920 #endif
1921 
1922  if (ctx->bluray_compat) {
1923  ctx->aud = 1;
1924  ctx->dpb_size = FFMIN(FFMAX(avctx->refs, 0), 6);
1925  avctx->max_b_frames = FFMIN(avctx->max_b_frames, 3);
1926  switch (avctx->codec->id) {
1927  case AV_CODEC_ID_H264:
1928  /* maximum level depends on used resolution */
1929  break;
1930  case AV_CODEC_ID_HEVC:
1931  ctx->level = NV_ENC_LEVEL_HEVC_51;
1932  ctx->tier = NV_ENC_TIER_HEVC_HIGH;
1933  break;
1934  }
1935  }
1936 
1937  if (avctx->gop_size > 0) {
1938  // only overwrite preset if a GOP size was selected as input
1939  ctx->encode_config.gopLength = avctx->gop_size;
1940  } else if (avctx->gop_size == 0) {
1941  ctx->encode_config.frameIntervalP = 0;
1942  ctx->encode_config.gopLength = 1;
1943  }
1944 
1945  if (avctx->max_b_frames >= 0 && ctx->encode_config.gopLength > 1) {
1946  /* 0 is intra-only, 1 is I/P only, 2 is one B-Frame, 3 two B-frames, and so on. */
1947  ctx->encode_config.frameIntervalP = avctx->max_b_frames + 1;
1948  }
1949 
1950  /* force to enable intra refresh */
1951  if(ctx->single_slice_intra_refresh)
1952  ctx->intra_refresh = 1;
1953 
1954  nvenc_recalc_surfaces(avctx);
1955 
1956  res = nvenc_setup_rate_control(avctx);
1957  if (res < 0)
1958  return res;
1959 
1960  if (avctx->flags & AV_CODEC_FLAG_INTERLACED_DCT) {
1961  ctx->encode_config.frameFieldMode = NV_ENC_PARAMS_FRAME_FIELD_MODE_FIELD;
1962  } else {
1963  ctx->encode_config.frameFieldMode = NV_ENC_PARAMS_FRAME_FIELD_MODE_FRAME;
1964  }
1965 
1966  res = nvenc_setup_codec_config(avctx);
1967  if (res)
1968  return res;
1969 
1970  res = nvenc_push_context(avctx);
1971  if (res < 0)
1972  return res;
1973 
1974  nv_status = p_nvenc->nvEncInitializeEncoder(ctx->nvencoder, &ctx->init_encode_params);
1975  if (nv_status != NV_ENC_SUCCESS) {
1976  nvenc_pop_context(avctx);
1977  return nvenc_print_error(avctx, nv_status, "InitializeEncoder failed");
1978  }
1979 
1980 #ifdef NVENC_HAVE_CUSTREAM_PTR
1981  if (ctx->cu_context) {
1982  nv_status = p_nvenc->nvEncSetIOCudaStreams(ctx->nvencoder, &ctx->cu_stream, &ctx->cu_stream);
1983  if (nv_status != NV_ENC_SUCCESS) {
1984  nvenc_pop_context(avctx);
1985  return nvenc_print_error(avctx, nv_status, "SetIOCudaStreams failed");
1986  }
1987  }
1988 #endif
1989 
1990  res = nvenc_pop_context(avctx);
1991  if (res < 0)
1992  return res;
1993 
1994  if (ctx->encode_config.frameIntervalP > 1)
1995  avctx->has_b_frames = 2;
1996 
1997  if (ctx->encode_config.rcParams.averageBitRate > 0)
1998  avctx->bit_rate = ctx->encode_config.rcParams.averageBitRate;
1999 
2000  cpb_props = ff_encode_add_cpb_side_data(avctx);
2001  if (!cpb_props)
2002  return AVERROR(ENOMEM);
2003  cpb_props->max_bitrate = ctx->encode_config.rcParams.maxBitRate;
2004  cpb_props->avg_bitrate = avctx->bit_rate;
2005  cpb_props->buffer_size = ctx->encode_config.rcParams.vbvBufferSize;
2006 
2007  return 0;
2008 }
2009 
2010 static NV_ENC_BUFFER_FORMAT nvenc_map_buffer_format(enum AVPixelFormat pix_fmt)
2011 {
2012  switch (pix_fmt) {
2013  case AV_PIX_FMT_YUV420P:
2014  return NV_ENC_BUFFER_FORMAT_YV12;
2015  case AV_PIX_FMT_NV12:
2016  return NV_ENC_BUFFER_FORMAT_NV12;
2017  case AV_PIX_FMT_P010:
2018  case AV_PIX_FMT_P016:
2019  return NV_ENC_BUFFER_FORMAT_YUV420_10BIT;
2020  case AV_PIX_FMT_GBRP:
2021  case AV_PIX_FMT_YUV444P:
2022  return NV_ENC_BUFFER_FORMAT_YUV444;
2023  case AV_PIX_FMT_GBRP16:
2024  case AV_PIX_FMT_GBRP10MSB:
2025  case AV_PIX_FMT_YUV444P16:
2026  case AV_PIX_FMT_YUV444P10MSB:
2027  return NV_ENC_BUFFER_FORMAT_YUV444_10BIT;
2028  case AV_PIX_FMT_0RGB32:
2029  case AV_PIX_FMT_RGB32:
2030  return NV_ENC_BUFFER_FORMAT_ARGB;
2031  case AV_PIX_FMT_0BGR32:
2032  case AV_PIX_FMT_BGR32:
2033  return NV_ENC_BUFFER_FORMAT_ABGR;
2034  case AV_PIX_FMT_X2RGB10:
2035  return NV_ENC_BUFFER_FORMAT_ARGB10;
2036  case AV_PIX_FMT_X2BGR10:
2037  return NV_ENC_BUFFER_FORMAT_ABGR10;
2038 #ifdef NVENC_HAVE_422_SUPPORT
2039  case AV_PIX_FMT_NV16:
2040  return NV_ENC_BUFFER_FORMAT_NV16;
2041  case AV_PIX_FMT_P210:
2042  case AV_PIX_FMT_P216:
2043  return NV_ENC_BUFFER_FORMAT_P210;
2044 #endif
2045  default:
2046  return NV_ENC_BUFFER_FORMAT_UNDEFINED;
2047  }
2048 }
2049 
2050 static av_cold int nvenc_alloc_surface(AVCodecContext *avctx, int idx)
2051 {
2052  NvencContext *ctx = avctx->priv_data;
2053  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
2054  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
2055  NvencSurface* tmp_surface = &ctx->surfaces[idx];
2056 
2057  NVENCSTATUS nv_status;
2058  NV_ENC_CREATE_BITSTREAM_BUFFER allocOut = { 0 };
2059  allocOut.version = NV_ENC_CREATE_BITSTREAM_BUFFER_VER;
2060 
2061  if (avctx->pix_fmt == AV_PIX_FMT_CUDA || avctx->pix_fmt == AV_PIX_FMT_D3D11) {
2062  ctx->surfaces[idx].in_ref = av_frame_alloc();
2063  if (!ctx->surfaces[idx].in_ref)
2064  return AVERROR(ENOMEM);
2065  } else {
2066  NV_ENC_CREATE_INPUT_BUFFER allocSurf = { 0 };
2067 
2068  ctx->surfaces[idx].format = nvenc_map_buffer_format(ctx->data_pix_fmt);
2069  if (ctx->surfaces[idx].format == NV_ENC_BUFFER_FORMAT_UNDEFINED) {
2070  av_log(avctx, AV_LOG_FATAL, "Invalid input pixel format: %s\n",
2071  av_get_pix_fmt_name(ctx->data_pix_fmt));
2072  return AVERROR(EINVAL);
2073  }
2074 
2075  allocSurf.version = NV_ENC_CREATE_INPUT_BUFFER_VER;
2076  allocSurf.width = avctx->width;
2077  allocSurf.height = avctx->height;
2078  allocSurf.bufferFmt = ctx->surfaces[idx].format;
2079 
2080  nv_status = p_nvenc->nvEncCreateInputBuffer(ctx->nvencoder, &allocSurf);
2081  if (nv_status != NV_ENC_SUCCESS) {
2082  return nvenc_print_error(avctx, nv_status, "CreateInputBuffer failed");
2083  }
2084 
2085  ctx->surfaces[idx].input_surface = allocSurf.inputBuffer;
2086  ctx->surfaces[idx].width = allocSurf.width;
2087  ctx->surfaces[idx].height = allocSurf.height;
2088  }
2089 
2090  nv_status = p_nvenc->nvEncCreateBitstreamBuffer(ctx->nvencoder, &allocOut);
2091  if (nv_status != NV_ENC_SUCCESS) {
2092  int err = nvenc_print_error(avctx, nv_status, "CreateBitstreamBuffer failed");
2093  if (avctx->pix_fmt != AV_PIX_FMT_CUDA && avctx->pix_fmt != AV_PIX_FMT_D3D11)
2094  p_nvenc->nvEncDestroyInputBuffer(ctx->nvencoder, ctx->surfaces[idx].input_surface);
2095  av_frame_free(&ctx->surfaces[idx].in_ref);
2096  return err;
2097  }
2098 
2099  ctx->surfaces[idx].output_surface = allocOut.bitstreamBuffer;
2100 
2101  av_fifo_write(ctx->unused_surface_queue, &tmp_surface, 1);
2102 
2103  return 0;
2104 }
2105 
2106 static av_cold int nvenc_setup_surfaces(AVCodecContext *avctx)
2107 {
2108  NvencContext *ctx = avctx->priv_data;
2109  int i, res = 0, res2;
2110 
2111  ctx->surfaces = av_calloc(ctx->nb_surfaces, sizeof(*ctx->surfaces));
2112  if (!ctx->surfaces)
2113  return AVERROR(ENOMEM);
2114 
2115  ctx->frame_data_array = av_calloc(ctx->frame_data_array_nb, sizeof(*ctx->frame_data_array));
2116  if (!ctx->frame_data_array)
2117  return AVERROR(ENOMEM);
2118 
2119  ctx->timestamp_list = av_fifo_alloc2(ctx->nb_surfaces + ctx->encode_config.frameIntervalP,
2120  sizeof(int64_t), 0);
2121  if (!ctx->timestamp_list)
2122  return AVERROR(ENOMEM);
2123 
2124  ctx->unused_surface_queue = av_fifo_alloc2(ctx->nb_surfaces, sizeof(NvencSurface*), 0);
2125  if (!ctx->unused_surface_queue)
2126  return AVERROR(ENOMEM);
2127 
2128  ctx->output_surface_queue = av_fifo_alloc2(ctx->nb_surfaces, sizeof(NvencSurface*), 0);
2129  if (!ctx->output_surface_queue)
2130  return AVERROR(ENOMEM);
2131  ctx->output_surface_ready_queue = av_fifo_alloc2(ctx->nb_surfaces, sizeof(NvencSurface*), 0);
2132  if (!ctx->output_surface_ready_queue)
2133  return AVERROR(ENOMEM);
2134 
2135  res = nvenc_push_context(avctx);
2136  if (res < 0)
2137  return res;
2138 
2139  for (i = 0; i < ctx->nb_surfaces; i++) {
2140  if ((res = nvenc_alloc_surface(avctx, i)) < 0)
2141  goto fail;
2142  }
2143 
2144 fail:
2145  res2 = nvenc_pop_context(avctx);
2146  if (res2 < 0)
2147  return res2;
2148 
2149  return res;
2150 }
2151 
2152 static av_cold int nvenc_setup_extradata(AVCodecContext *avctx)
2153 {
2154  NvencContext *ctx = avctx->priv_data;
2155  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
2156  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
2157 
2158  NVENCSTATUS nv_status;
2159  uint32_t outSize = 0;
2160  char tmpHeader[NV_MAX_SEQ_HDR_LEN];
2161 
2162  NV_ENC_SEQUENCE_PARAM_PAYLOAD payload = { 0 };
2163  payload.version = NV_ENC_SEQUENCE_PARAM_PAYLOAD_VER;
2164 
2165  payload.spsppsBuffer = tmpHeader;
2166  payload.inBufferSize = sizeof(tmpHeader);
2167  payload.outSPSPPSPayloadSize = &outSize;
2168 
2169  nv_status = p_nvenc->nvEncGetSequenceParams(ctx->nvencoder, &payload);
2170  if (nv_status != NV_ENC_SUCCESS) {
2171  return nvenc_print_error(avctx, nv_status, "GetSequenceParams failed");
2172  }
2173 
2174  avctx->extradata_size = outSize;
2175  avctx->extradata = av_mallocz(outSize + AV_INPUT_BUFFER_PADDING_SIZE);
2176 
2177  if (!avctx->extradata) {
2178  return AVERROR(ENOMEM);
2179  }
2180 
2181  memcpy(avctx->extradata, tmpHeader, outSize);
2182 
2183  return 0;
2184 }
2185 
2186 av_cold int ff_nvenc_encode_close(AVCodecContext *avctx)
2187 {
2188  NvencContext *ctx = avctx->priv_data;
2189  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
2190  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
2191  int i, res;
2192 
2193  /* the encoder has to be flushed before it can be closed */
2194  if (ctx->nvencoder) {
2195  NV_ENC_PIC_PARAMS params = { .version = NV_ENC_PIC_PARAMS_VER,
2196  .encodePicFlags = NV_ENC_PIC_FLAG_EOS };
2197 
2198  res = nvenc_push_context(avctx);
2199  if (res < 0)
2200  return res;
2201 
2202  p_nvenc->nvEncEncodePicture(ctx->nvencoder, &params);
2203  }
2204 
2205  av_fifo_freep2(&ctx->timestamp_list);
2206  av_fifo_freep2(&ctx->output_surface_ready_queue);
2207  av_fifo_freep2(&ctx->output_surface_queue);
2208  av_fifo_freep2(&ctx->unused_surface_queue);
2209 
2210  if (ctx->frame_data_array) {
2211  for (i = 0; i < ctx->frame_data_array_nb; i++)
2212  av_buffer_unref(&ctx->frame_data_array[i].frame_opaque_ref);
2213  av_freep(&ctx->frame_data_array);
2214  }
2215 
2216  if (ctx->surfaces && (avctx->pix_fmt == AV_PIX_FMT_CUDA || avctx->pix_fmt == AV_PIX_FMT_D3D11)) {
2217  for (i = 0; i < ctx->nb_registered_frames; i++) {
2218  if (ctx->registered_frames[i].mapped)
2219  p_nvenc->nvEncUnmapInputResource(ctx->nvencoder, ctx->registered_frames[i].in_map.mappedResource);
2220  if (ctx->registered_frames[i].regptr)
2221  p_nvenc->nvEncUnregisterResource(ctx->nvencoder, ctx->registered_frames[i].regptr);
2222  }
2223  ctx->nb_registered_frames = 0;
2224  }
2225 
2226  if (ctx->surfaces) {
2227  for (i = 0; i < ctx->nb_surfaces; ++i) {
2228  if (avctx->pix_fmt != AV_PIX_FMT_CUDA && avctx->pix_fmt != AV_PIX_FMT_D3D11)
2229  p_nvenc->nvEncDestroyInputBuffer(ctx->nvencoder, ctx->surfaces[i].input_surface);
2230  av_frame_free(&ctx->surfaces[i].in_ref);
2231  p_nvenc->nvEncDestroyBitstreamBuffer(ctx->nvencoder, ctx->surfaces[i].output_surface);
2232  }
2233  }
2234  av_freep(&ctx->surfaces);
2235  ctx->nb_surfaces = 0;
2236 
2237  av_frame_free(&ctx->frame);
2238 
2239  av_freep(&ctx->sei_data);
2240 
2241  if (ctx->nvencoder) {
2242  p_nvenc->nvEncDestroyEncoder(ctx->nvencoder);
2243 
2244  res = nvenc_pop_context(avctx);
2245  if (res < 0)
2246  return res;
2247  }
2248  ctx->nvencoder = NULL;
2249 
2250  if (ctx->cu_context_internal)
2251  CHECK_CU(dl_fn->cuda_dl->cuCtxDestroy(ctx->cu_context_internal));
2252  ctx->cu_context = ctx->cu_context_internal = NULL;
2253 
2254 #if CONFIG_D3D11VA
2255  if (ctx->d3d11_device) {
2256  ID3D11Device_Release(ctx->d3d11_device);
2257  ctx->d3d11_device = NULL;
2258  }
2259 #endif
2260 
2261  nvenc_free_functions(&dl_fn->nvenc_dl);
2262  cuda_free_functions(&dl_fn->cuda_dl);
2263 
2264  dl_fn->nvenc_device_count = 0;
2265 
2266  av_log(avctx, AV_LOG_VERBOSE, "Nvenc unloaded\n");
2267 
2268  return 0;
2269 }
2270 
2271 av_cold int ff_nvenc_encode_init(AVCodecContext *avctx)
2272 {
2273  NvencContext *ctx = avctx->priv_data;
2274  int ret;
2275 
2276  if (avctx->pix_fmt == AV_PIX_FMT_CUDA || avctx->pix_fmt == AV_PIX_FMT_D3D11) {
2277  AVHWFramesContext *frames_ctx;
2278  if (!avctx->hw_frames_ctx) {
2279  av_log(avctx, AV_LOG_ERROR,
2280  "hw_frames_ctx must be set when using GPU frames as input\n");
2281  return AVERROR(EINVAL);
2282  }
2283  frames_ctx = (AVHWFramesContext*)avctx->hw_frames_ctx->data;
2284  if (frames_ctx->format != avctx->pix_fmt) {
2285  av_log(avctx, AV_LOG_ERROR,
2286  "hw_frames_ctx must match the GPU frame type\n");
2287  return AVERROR(EINVAL);
2288  }
2289  ctx->data_pix_fmt = frames_ctx->sw_format;
2290  } else {
2291  ctx->data_pix_fmt = avctx->pix_fmt;
2292  }
2293 
2294  if (ctx->rgb_mode == NVENC_RGB_MODE_DISABLED && IS_RGB(ctx->data_pix_fmt)) {
2295  av_log(avctx, AV_LOG_ERROR, "Packed RGB input, but RGB support is disabled.\n");
2296  return AVERROR(EINVAL);
2297  }
2298 
2299  ctx->frame = av_frame_alloc();
2300  if (!ctx->frame)
2301  return AVERROR(ENOMEM);
2302 
2303  if ((ret = nvenc_load_libraries(avctx)) < 0)
2304  return ret;
2305 
2306  if ((ret = nvenc_setup_device(avctx)) < 0)
2307  return ret;
2308 
2309  if ((ret = nvenc_setup_encoder(avctx)) < 0)
2310  return ret;
2311 
2312  if ((ret = nvenc_setup_surfaces(avctx)) < 0)
2313  return ret;
2314 
2315  if (avctx->flags & AV_CODEC_FLAG_GLOBAL_HEADER) {
2316  if ((ret = nvenc_setup_extradata(avctx)) < 0)
2317  return ret;
2318  }
2319 
2320  return 0;
2321 }
2322 
2323 static NvencSurface *get_free_frame(NvencContext *ctx)
2324 {
2325  NvencSurface *tmp_surf;
2326 
2327  if (av_fifo_read(ctx->unused_surface_queue, &tmp_surf, 1) < 0)
2328  // queue empty
2329  return NULL;
2330 
2331  return tmp_surf;
2332 }
2333 
2334 static int nvenc_copy_frame(AVCodecContext *avctx, NvencSurface *nv_surface,
2335  NV_ENC_LOCK_INPUT_BUFFER *lock_buffer_params, const AVFrame *frame)
2336 {
2337  int dst_linesize[4] = {
2338  lock_buffer_params->pitch,
2339  lock_buffer_params->pitch,
2340  lock_buffer_params->pitch,
2341  lock_buffer_params->pitch
2342  };
2343  uint8_t *dst_data[4];
2344  int ret;
2345 
2346  if (frame->format == AV_PIX_FMT_YUV420P)
2347  dst_linesize[1] = dst_linesize[2] >>= 1;
2348 
2349  ret = av_image_fill_pointers(dst_data, frame->format, nv_surface->height,
2350  lock_buffer_params->bufferDataPtr, dst_linesize);
2351  if (ret < 0)
2352  return ret;
2353 
2354  if (frame->format == AV_PIX_FMT_YUV420P)
2355  FFSWAP(uint8_t*, dst_data[1], dst_data[2]);
2356 
2357  av_image_copy2(dst_data, dst_linesize,
2358  frame->data, frame->linesize, frame->format,
2359  avctx->width, avctx->height);
2360 
2361  return 0;
2362 }
2363 
2364 static int nvenc_find_free_reg_resource(AVCodecContext *avctx)
2365 {
2366  NvencContext *ctx = avctx->priv_data;
2367  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
2368  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
2369  NVENCSTATUS nv_status;
2370 
2371  int i, first_round;
2372 
2373  if (ctx->nb_registered_frames == FF_ARRAY_ELEMS(ctx->registered_frames)) {
2374  for (first_round = 1; first_round >= 0; first_round--) {
2375  for (i = 0; i < ctx->nb_registered_frames; i++) {
2376  if (!ctx->registered_frames[i].mapped) {
2377  if (ctx->registered_frames[i].regptr) {
2378  if (first_round)
2379  continue;
2380  nv_status = p_nvenc->nvEncUnregisterResource(ctx->nvencoder, ctx->registered_frames[i].regptr);
2381  if (nv_status != NV_ENC_SUCCESS)
2382  return nvenc_print_error(avctx, nv_status, "Failed unregistering unused input resource");
2383  ctx->registered_frames[i].ptr = NULL;
2384  ctx->registered_frames[i].regptr = NULL;
2385  }
2386  return i;
2387  }
2388  }
2389  }
2390  } else {
2391  return ctx->nb_registered_frames++;
2392  }
2393 
2394  av_log(avctx, AV_LOG_ERROR, "Too many registered CUDA frames\n");
2395  return AVERROR(ENOMEM);
2396 }
2397 
2398 static int nvenc_register_frame(AVCodecContext *avctx, const AVFrame *frame)
2399 {
2400  NvencContext *ctx = avctx->priv_data;
2401  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
2402  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
2403 
2404  AVHWFramesContext *frames_ctx = (AVHWFramesContext*)frame->hw_frames_ctx->data;
2405  NV_ENC_REGISTER_RESOURCE reg = { 0 };
2406  int i, idx, ret;
2407 
2408  for (i = 0; i < ctx->nb_registered_frames; i++) {
2409  if (avctx->pix_fmt == AV_PIX_FMT_CUDA && ctx->registered_frames[i].ptr == frame->data[0])
2410  return i;
2411  else if (avctx->pix_fmt == AV_PIX_FMT_D3D11 && ctx->registered_frames[i].ptr == frame->data[0] && ctx->registered_frames[i].ptr_index == (intptr_t)frame->data[1])
2412  return i;
2413  }
2414 
2415  idx = nvenc_find_free_reg_resource(avctx);
2416  if (idx < 0)
2417  return idx;
2418 
2419  reg.version = NV_ENC_REGISTER_RESOURCE_VER;
2420  reg.width = frames_ctx->width;
2421  reg.height = frames_ctx->height;
2422  reg.pitch = frame->linesize[0];
2423  reg.resourceToRegister = frame->data[0];
2424 
2425  if (avctx->pix_fmt == AV_PIX_FMT_CUDA) {
2426  reg.resourceType = NV_ENC_INPUT_RESOURCE_TYPE_CUDADEVICEPTR;
2427  }
2428  else if (avctx->pix_fmt == AV_PIX_FMT_D3D11) {
2429  reg.resourceType = NV_ENC_INPUT_RESOURCE_TYPE_DIRECTX;
2430  reg.subResourceIndex = (intptr_t)frame->data[1];
2431  }
2432 
2433  reg.bufferFormat = nvenc_map_buffer_format(frames_ctx->sw_format);
2434  if (reg.bufferFormat == NV_ENC_BUFFER_FORMAT_UNDEFINED) {
2435  av_log(avctx, AV_LOG_FATAL, "Invalid input pixel format: %s\n",
2436  av_get_pix_fmt_name(frames_ctx->sw_format));
2437  return AVERROR(EINVAL);
2438  }
2439 
2440  ret = p_nvenc->nvEncRegisterResource(ctx->nvencoder, &reg);
2441  if (ret != NV_ENC_SUCCESS) {
2442  nvenc_print_error(avctx, ret, "Error registering an input resource");
2443  return AVERROR_UNKNOWN;
2444  }
2445 
2446  ctx->registered_frames[idx].ptr = frame->data[0];
2447  ctx->registered_frames[idx].ptr_index = reg.subResourceIndex;
2448  ctx->registered_frames[idx].regptr = reg.registeredResource;
2449  return idx;
2450 }
2451 
2452 static int nvenc_upload_frame(AVCodecContext *avctx, const AVFrame *frame,
2453  NvencSurface *nvenc_frame)
2454 {
2455  NvencContext *ctx = avctx->priv_data;
2456  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
2457  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
2458 
2459  int res;
2460  NVENCSTATUS nv_status;
2461 
2462  if (avctx->pix_fmt == AV_PIX_FMT_CUDA || avctx->pix_fmt == AV_PIX_FMT_D3D11) {
2463  int reg_idx = nvenc_register_frame(avctx, frame);
2464  if (reg_idx < 0) {
2465  av_log(avctx, AV_LOG_ERROR, "Could not register an input HW frame\n");
2466  return reg_idx;
2467  }
2468 
2469  res = av_frame_ref(nvenc_frame->in_ref, frame);
2470  if (res < 0)
2471  return res;
2472 
2473  if (!ctx->registered_frames[reg_idx].mapped) {
2474  ctx->registered_frames[reg_idx].in_map.version = NV_ENC_MAP_INPUT_RESOURCE_VER;
2475  ctx->registered_frames[reg_idx].in_map.registeredResource = ctx->registered_frames[reg_idx].regptr;
2476  nv_status = p_nvenc->nvEncMapInputResource(ctx->nvencoder, &ctx->registered_frames[reg_idx].in_map);
2477  if (nv_status != NV_ENC_SUCCESS) {
2478  av_frame_unref(nvenc_frame->in_ref);
2479  return nvenc_print_error(avctx, nv_status, "Error mapping an input resource");
2480  }
2481  }
2482 
2483  ctx->registered_frames[reg_idx].mapped += 1;
2484 
2485  nvenc_frame->reg_idx = reg_idx;
2486  nvenc_frame->input_surface = ctx->registered_frames[reg_idx].in_map.mappedResource;
2487  nvenc_frame->format = ctx->registered_frames[reg_idx].in_map.mappedBufferFmt;
2488  nvenc_frame->pitch = frame->linesize[0];
2489 
2490  return 0;
2491  } else {
2492  NV_ENC_LOCK_INPUT_BUFFER lockBufferParams = { 0 };
2493 
2494  lockBufferParams.version = NV_ENC_LOCK_INPUT_BUFFER_VER;
2495  lockBufferParams.inputBuffer = nvenc_frame->input_surface;
2496 
2497  nv_status = p_nvenc->nvEncLockInputBuffer(ctx->nvencoder, &lockBufferParams);
2498  if (nv_status != NV_ENC_SUCCESS) {
2499  return nvenc_print_error(avctx, nv_status, "Failed locking nvenc input buffer");
2500  }
2501 
2502  nvenc_frame->pitch = lockBufferParams.pitch;
2503  res = nvenc_copy_frame(avctx, nvenc_frame, &lockBufferParams, frame);
2504 
2505  nv_status = p_nvenc->nvEncUnlockInputBuffer(ctx->nvencoder, nvenc_frame->input_surface);
2506  if (nv_status != NV_ENC_SUCCESS) {
2507  return nvenc_print_error(avctx, nv_status, "Failed unlocking input buffer!");
2508  }
2509 
2510  return res;
2511  }
2512 }
2513 
2514 #ifdef NVENC_HAVE_TIME_CODE
2515 static void nvenc_fill_time_code(AVCodecContext *avctx, const AVFrame *frame, NV_ENC_TIME_CODE *time_code)
2516 {
2517  AVFrameSideData *sd = av_frame_get_side_data(frame, AV_FRAME_DATA_S12M_TIMECODE);
2518 
2519  if (sd) {
2520  uint32_t *tc = (uint32_t*)sd->data;
2521  int cnt = FFMIN(tc[0], FF_ARRAY_ELEMS(time_code->clockTimestamp));
2522 
2523  switch (cnt) {
2524  case 0:
2525  time_code->displayPicStruct = NV_ENC_PIC_STRUCT_DISPLAY_FRAME;
2526  time_code->skipClockTimestampInsertion = 1;
2527  break;
2528  case 2:
2529  time_code->displayPicStruct = NV_ENC_PIC_STRUCT_DISPLAY_FRAME_DOUBLING;
2530  break;
2531  case 3:
2532  time_code->displayPicStruct = NV_ENC_PIC_STRUCT_DISPLAY_FRAME_TRIPLING;
2533  break;
2534  default:
2535  time_code->displayPicStruct = NV_ENC_PIC_STRUCT_DISPLAY_FRAME;
2536  break;
2537  }
2538 
2539  for (int i = 0; i < cnt; i++) {
2540  unsigned hh, mm, ss, ff, drop;
2541  ff_timecode_set_smpte(&drop, &hh, &mm, &ss, &ff, avctx->framerate, tc[i + 1], 0, 0);
2542 
2543  time_code->clockTimestamp[i].countingType = 0;
2544  time_code->clockTimestamp[i].discontinuityFlag = 0;
2545  time_code->clockTimestamp[i].cntDroppedFrames = drop;
2546  time_code->clockTimestamp[i].nFrames = ff;
2547  time_code->clockTimestamp[i].secondsValue = ss;
2548  time_code->clockTimestamp[i].minutesValue = mm;
2549  time_code->clockTimestamp[i].hoursValue = hh;
2550  time_code->clockTimestamp[i].timeOffset = 0;
2551  }
2552  } else {
2553  time_code->displayPicStruct = NV_ENC_PIC_STRUCT_DISPLAY_FRAME;
2554  time_code->skipClockTimestampInsertion = 1;
2555  }
2556 }
2557 #endif
2558 
2559 static void nvenc_codec_specific_pic_params(AVCodecContext *avctx, const AVFrame *frame,
2560  NV_ENC_PIC_PARAMS *params,
2561  NV_ENC_SEI_PAYLOAD *sei_data,
2562  int sei_count)
2563 {
2564  NvencContext *ctx = avctx->priv_data;
2565 
2566  switch (avctx->codec->id) {
2567  case AV_CODEC_ID_H264:
2568  params->codecPicParams.h264PicParams.sliceMode =
2569  ctx->encode_config.encodeCodecConfig.h264Config.sliceMode;
2570  params->codecPicParams.h264PicParams.sliceModeData =
2571  ctx->encode_config.encodeCodecConfig.h264Config.sliceModeData;
2572  if (sei_count > 0) {
2573  params->codecPicParams.h264PicParams.seiPayloadArray = sei_data;
2574  params->codecPicParams.h264PicParams.seiPayloadArrayCnt = sei_count;
2575  }
2576 
2577 #ifdef NVENC_HAVE_TIME_CODE
2578  if (ctx->s12m_tc)
2579  nvenc_fill_time_code(avctx, frame, &params->codecPicParams.h264PicParams.timeCode);
2580 #endif
2581 
2582  break;
2583  case AV_CODEC_ID_HEVC:
2584  params->codecPicParams.hevcPicParams.sliceMode =
2585  ctx->encode_config.encodeCodecConfig.hevcConfig.sliceMode;
2586  params->codecPicParams.hevcPicParams.sliceModeData =
2587  ctx->encode_config.encodeCodecConfig.hevcConfig.sliceModeData;
2588  if (sei_count > 0) {
2589  params->codecPicParams.hevcPicParams.seiPayloadArray = sei_data;
2590  params->codecPicParams.hevcPicParams.seiPayloadArrayCnt = sei_count;
2591  }
2592 
2593  break;
2594 #if CONFIG_AV1_NVENC_ENCODER
2595  case AV_CODEC_ID_AV1:
2596  params->codecPicParams.av1PicParams.numTileColumns =
2597  ctx->encode_config.encodeCodecConfig.av1Config.numTileColumns;
2598  params->codecPicParams.av1PicParams.numTileRows =
2599  ctx->encode_config.encodeCodecConfig.av1Config.numTileRows;
2600  if (sei_count > 0) {
2601  params->codecPicParams.av1PicParams.obuPayloadArray = sei_data;
2602  params->codecPicParams.av1PicParams.obuPayloadArrayCnt = sei_count;
2603  }
2604 
2605  break;
2606 #endif
2607  }
2608 }
2609 
2610 static inline void timestamp_queue_enqueue(AVFifo *queue, int64_t timestamp)
2611 {
2612  av_fifo_write(queue, &timestamp, 1);
2613 }
2614 
2615 static inline int64_t timestamp_queue_dequeue(AVFifo *queue)
2616 {
2617  int64_t timestamp = AV_NOPTS_VALUE;
2618  // The following call might fail if the queue is empty.
2619  av_fifo_read(queue, &timestamp, 1);
2620 
2621  return timestamp;
2622 }
2623 
2624 static inline int64_t timestamp_queue_peek(AVFifo *queue, size_t index)
2625 {
2626  int64_t timestamp = AV_NOPTS_VALUE;
2627  av_fifo_peek(queue, &timestamp, 1, index);
2628 
2629  return timestamp;
2630 }
2631 
2632 static int nvenc_set_timestamp(AVCodecContext *avctx,
2633  NV_ENC_LOCK_BITSTREAM *params,
2634  AVPacket *pkt)
2635 {
2636  NvencContext *ctx = avctx->priv_data;
2637  unsigned int delay;
2638  int64_t delay_time;
2639 
2640  pkt->pts = params->outputTimeStamp;
2641 
2642  if (!(avctx->codec_descriptor->props & AV_CODEC_PROP_REORDER)) {
2643  pkt->dts = pkt->pts;
2644  return 0;
2645  }
2646 
2647  // This can be more than necessary, but we don't know the real reorder delay.
2648  delay = FFMAX(ctx->encode_config.frameIntervalP - 1, 0);
2649 #ifdef NVENC_HAVE_MVHEVC
2650  delay *= ctx->multiview ? 2 : 1;
2651 #endif
2652  if (ctx->output_frame_num >= delay) {
2653  pkt->dts = timestamp_queue_dequeue(ctx->timestamp_list);
2654  ctx->output_frame_num++;
2655  return 0;
2656  }
2657 
2658  delay_time = ctx->initial_delay_time;
2659  if (!delay_time) {
2660  int64_t t1, t2, t3;
2661  t1 = timestamp_queue_peek(ctx->timestamp_list, delay);
2662  t2 = timestamp_queue_peek(ctx->timestamp_list, 0);
2663  t3 = (delay > 1) ? timestamp_queue_peek(ctx->timestamp_list, 1) : t1;
2664 
2665  if (t1 != AV_NOPTS_VALUE) {
2666  delay_time = t1 - t2;
2667  } else if (avctx->framerate.num > 0 && avctx->framerate.den > 0) {
2668  delay_time = av_rescale_q(delay, (AVRational) {avctx->framerate.den, avctx->framerate.num},
2669  avctx->time_base);
2670  } else if (t3 != AV_NOPTS_VALUE) {
2671  delay_time = delay * (t3 - t2);
2672  } else {
2673  delay_time = delay;
2674  }
2675  ctx->initial_delay_time = delay_time;
2676  }
2677 
2678  /* The following method is simple, but doesn't guarantee monotonic with VFR
2679  * when delay_time isn't accurate (that is, t1 == AV_NOPTS_VALUE)
2680  *
2681  * dts = timestamp_queue_peek(ctx->timestamp_list, ctx->output_frame_num) - delay_time
2682  */
2683  pkt->dts = timestamp_queue_peek(ctx->timestamp_list, 0) - delay_time * (delay - ctx->output_frame_num) / delay;
2684  ctx->output_frame_num++;
2685 
2686  return 0;
2687 }
2688 
2689 static int nvenc_store_frame_data(AVCodecContext *avctx, NV_ENC_PIC_PARAMS *pic_params, const AVFrame *frame)
2690 {
2691  NvencContext *ctx = avctx->priv_data;
2692  int res = 0;
2693 
2694  int idx = ctx->frame_data_array_pos;
2695  NvencFrameData *frame_data = &ctx->frame_data_array[idx];
2696 
2697  // in case the encoder got reconfigured, there might be leftovers
2698  av_buffer_unref(&frame_data->frame_opaque_ref);
2699 
2700  if (frame->opaque_ref && avctx->flags & AV_CODEC_FLAG_COPY_OPAQUE) {
2701  frame_data->frame_opaque_ref = av_buffer_ref(frame->opaque_ref);
2702  if (!frame_data->frame_opaque_ref)
2703  return AVERROR(ENOMEM);
2704  }
2705 
2706  frame_data->duration = frame->duration;
2707  frame_data->frame_opaque = frame->opaque;
2708 
2709  ctx->frame_data_array_pos = (ctx->frame_data_array_pos + 1) % ctx->frame_data_array_nb;
2710  pic_params->inputDuration = idx;
2711 
2712  return res;
2713 }
2714 
2715 static int nvenc_retrieve_frame_data(AVCodecContext *avctx, NV_ENC_LOCK_BITSTREAM *lock_params, AVPacket *pkt)
2716 {
2717  NvencContext *ctx = avctx->priv_data;
2718  int res = 0;
2719 
2720  int idx = lock_params->outputDuration;
2721  NvencFrameData *frame_data = &ctx->frame_data_array[idx];
2722 
2723  pkt->duration = frame_data->duration;
2724 
2725  if (avctx->flags & AV_CODEC_FLAG_COPY_OPAQUE) {
2726  pkt->opaque = frame_data->frame_opaque;
2727  pkt->opaque_ref = frame_data->frame_opaque_ref;
2728  frame_data->frame_opaque_ref = NULL;
2729  }
2730 
2731  av_buffer_unref(&frame_data->frame_opaque_ref);
2732 
2733  return res;
2734 }
2735 
2736 static int process_output_surface(AVCodecContext *avctx, AVPacket *pkt, NvencSurface *tmpoutsurf)
2737 {
2738  NvencContext *ctx = avctx->priv_data;
2739  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
2740  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
2741 
2742  NV_ENC_LOCK_BITSTREAM lock_params = { 0 };
2743  NVENCSTATUS nv_status;
2744  int res = 0;
2745 
2746  enum AVPictureType pict_type;
2747 
2748  lock_params.version = NV_ENC_LOCK_BITSTREAM_VER;
2749 
2750  lock_params.doNotWait = 0;
2751  lock_params.outputBitstream = tmpoutsurf->output_surface;
2752 
2753  nv_status = p_nvenc->nvEncLockBitstream(ctx->nvencoder, &lock_params);
2754  if (nv_status != NV_ENC_SUCCESS) {
2755  res = nvenc_print_error(avctx, nv_status, "Failed locking bitstream buffer");
2756  goto error;
2757  }
2758 
2759  res = ff_get_encode_buffer(avctx, pkt, lock_params.bitstreamSizeInBytes, 0);
2760 
2761  if (res < 0) {
2762  p_nvenc->nvEncUnlockBitstream(ctx->nvencoder, tmpoutsurf->output_surface);
2763  goto error;
2764  }
2765 
2766  memcpy(pkt->data, lock_params.bitstreamBufferPtr, lock_params.bitstreamSizeInBytes);
2767 
2768  nv_status = p_nvenc->nvEncUnlockBitstream(ctx->nvencoder, tmpoutsurf->output_surface);
2769  if (nv_status != NV_ENC_SUCCESS) {
2770  res = nvenc_print_error(avctx, nv_status, "Failed unlocking bitstream buffer, expect the gates of mordor to open");
2771  goto error;
2772  }
2773 
2774 
2775  if (avctx->pix_fmt == AV_PIX_FMT_CUDA || avctx->pix_fmt == AV_PIX_FMT_D3D11) {
2776  ctx->registered_frames[tmpoutsurf->reg_idx].mapped -= 1;
2777  if (ctx->registered_frames[tmpoutsurf->reg_idx].mapped == 0) {
2778  nv_status = p_nvenc->nvEncUnmapInputResource(ctx->nvencoder, ctx->registered_frames[tmpoutsurf->reg_idx].in_map.mappedResource);
2779  if (nv_status != NV_ENC_SUCCESS) {
2780  res = nvenc_print_error(avctx, nv_status, "Failed unmapping input resource");
2781  goto error;
2782  }
2783  } else if (ctx->registered_frames[tmpoutsurf->reg_idx].mapped < 0) {
2784  res = AVERROR_BUG;
2785  goto error;
2786  }
2787 
2788  av_frame_unref(tmpoutsurf->in_ref);
2789 
2790  tmpoutsurf->input_surface = NULL;
2791  }
2792 
2793  switch (lock_params.pictureType) {
2794  case NV_ENC_PIC_TYPE_IDR:
2795  pkt->flags |= AV_PKT_FLAG_KEY;
2796  av_fallthrough;
2797  case NV_ENC_PIC_TYPE_I:
2798  pict_type = AV_PICTURE_TYPE_I;
2799  break;
2800  case NV_ENC_PIC_TYPE_P:
2801  pict_type = AV_PICTURE_TYPE_P;
2802  break;
2803  case NV_ENC_PIC_TYPE_B:
2804  pict_type = AV_PICTURE_TYPE_B;
2805  break;
2806  case NV_ENC_PIC_TYPE_BI:
2807  pict_type = AV_PICTURE_TYPE_BI;
2808  break;
2809  default:
2810  av_log(avctx, AV_LOG_ERROR, "Unknown picture type encountered, expect the output to be broken.\n");
2811  av_log(avctx, AV_LOG_ERROR, "Please report this error and include as much information on how to reproduce it as possible.\n");
2812  res = AVERROR_EXTERNAL;
2813  goto error;
2814  }
2815 
2816  ff_encode_add_stats_side_data(pkt,
2817  (lock_params.frameAvgQP - 1) * FF_QP2LAMBDA, NULL, 0, pict_type);
2818 
2819  res = nvenc_set_timestamp(avctx, &lock_params, pkt);
2820  if (res < 0)
2821  goto error2;
2822 
2823  res = nvenc_retrieve_frame_data(avctx, &lock_params, pkt);
2824  if (res < 0)
2825  goto error2;
2826 
2827  return 0;
2828 
2829 error:
2830  timestamp_queue_dequeue(ctx->timestamp_list);
2831 
2832 error2:
2833  return res;
2834 }
2835 
2836 static int output_ready(AVCodecContext *avctx, int flush)
2837 {
2838  NvencContext *ctx = avctx->priv_data;
2839  int nb_ready, nb_pending;
2840 
2841  nb_ready = av_fifo_can_read(ctx->output_surface_ready_queue);
2842  nb_pending = av_fifo_can_read(ctx->output_surface_queue);
2843  if (flush)
2844  return nb_ready > 0;
2845  return (nb_ready > 0) && (nb_ready + nb_pending >= ctx->async_depth);
2846 }
2847 
2848 static int prepare_sei_data_array(AVCodecContext *avctx, const AVFrame *frame)
2849 {
2850  NvencContext *ctx = avctx->priv_data;
2851  int sei_count = 0;
2852  int i, res;
2853 
2854  if (ctx->a53_cc && av_frame_get_side_data(frame, AV_FRAME_DATA_A53_CC)) {
2855  void *a53_data = NULL;
2856  size_t a53_size = 0;
2857 
2858  if (ff_alloc_a53_sei(frame, 0, &a53_data, &a53_size) < 0) {
2859  av_log(ctx, AV_LOG_ERROR, "Not enough memory for closed captions, skipping\n");
2860  }
2861 
2862  if (a53_data) {
2863  void *tmp = av_fast_realloc(ctx->sei_data,
2864  &ctx->sei_data_size,
2865  (sei_count + 1) * sizeof(*ctx->sei_data));
2866  if (!tmp) {
2867  av_free(a53_data);
2868  res = AVERROR(ENOMEM);
2869  goto error;
2870  } else {
2871  ctx->sei_data = tmp;
2872  ctx->sei_data[sei_count].payloadSize = (uint32_t)a53_size;
2873  ctx->sei_data[sei_count].payload = (uint8_t*)a53_data;
2874 
2875 #if CONFIG_AV1_NVENC_ENCODER
2876  if (avctx->codec->id == AV_CODEC_ID_AV1)
2877  ctx->sei_data[sei_count].payloadType = AV1_METADATA_TYPE_ITUT_T35;
2878  else
2879 #endif
2880  ctx->sei_data[sei_count].payloadType = SEI_TYPE_USER_DATA_REGISTERED_ITU_T_T35;
2881 
2882  sei_count++;
2883  }
2884  }
2885  }
2886 
2887  if (ctx->s12m_tc && avctx->codec->id != AV_CODEC_ID_H264 && av_frame_get_side_data(frame, AV_FRAME_DATA_S12M_TIMECODE)) {
2888  void *tc_data = NULL;
2889  size_t tc_size = 0;
2890 
2891  if (ff_alloc_timecode_sei(frame, avctx->framerate, 0, &tc_data, &tc_size) < 0) {
2892  av_log(ctx, AV_LOG_ERROR, "Not enough memory for timecode sei, skipping\n");
2893  }
2894 
2895  if (tc_data) {
2896  void *tmp = av_fast_realloc(ctx->sei_data,
2897  &ctx->sei_data_size,
2898  (sei_count + 1) * sizeof(*ctx->sei_data));
2899  if (!tmp) {
2900  av_free(tc_data);
2901  res = AVERROR(ENOMEM);
2902  goto error;
2903  } else {
2904  ctx->sei_data = tmp;
2905  ctx->sei_data[sei_count].payloadSize = (uint32_t)tc_size;
2906  ctx->sei_data[sei_count].payload = (uint8_t*)tc_data;
2907 
2908 #if CONFIG_AV1_NVENC_ENCODER
2909  if (avctx->codec->id == AV_CODEC_ID_AV1)
2910  ctx->sei_data[sei_count].payloadType = AV1_METADATA_TYPE_TIMECODE;
2911  else
2912 #endif
2913  ctx->sei_data[sei_count].payloadType = SEI_TYPE_TIME_CODE;
2914 
2915  sei_count++;
2916  }
2917  }
2918  }
2919 
2920  if (!ctx->udu_sei)
2921  return sei_count;
2922 
2923  for (i = 0; i < frame->nb_side_data; i++) {
2924  AVFrameSideData *side_data = frame->side_data[i];
2925  void *tmp;
2926 
2927  if (side_data->type != AV_FRAME_DATA_SEI_UNREGISTERED)
2928  continue;
2929 
2930  tmp = av_fast_realloc(ctx->sei_data,
2931  &ctx->sei_data_size,
2932  (sei_count + 1) * sizeof(*ctx->sei_data));
2933  if (!tmp) {
2934  res = AVERROR(ENOMEM);
2935  goto error;
2936  } else {
2937  ctx->sei_data = tmp;
2938  ctx->sei_data[sei_count].payloadSize = side_data->size;
2939  ctx->sei_data[sei_count].payloadType = SEI_TYPE_USER_DATA_UNREGISTERED;
2940  ctx->sei_data[sei_count].payload = av_memdup(side_data->data, side_data->size);
2941 
2942  if (!ctx->sei_data[sei_count].payload) {
2943  res = AVERROR(ENOMEM);
2944  goto error;
2945  }
2946 
2947  sei_count++;
2948  }
2949  }
2950 
2951  return sei_count;
2952 
2953 error:
2954  for (i = 0; i < sei_count; i++)
2955  av_freep(&(ctx->sei_data[i].payload));
2956 
2957  return res;
2958 }
2959 
2960 static void reconfig_encoder(AVCodecContext *avctx, const AVFrame *frame)
2961 {
2962  NvencContext *ctx = avctx->priv_data;
2963  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &ctx->nvenc_dload_funcs.nvenc_funcs;
2964  NVENCSTATUS ret;
2965 
2966  NV_ENC_RECONFIGURE_PARAMS params = { 0 };
2967  int needs_reconfig = 0;
2968  int needs_encode_config = 0;
2969  int reconfig_bitrate = 0, reconfig_dar = 0;
2970  int dw, dh;
2971 
2972  params.version = NV_ENC_RECONFIGURE_PARAMS_VER;
2973  params.reInitEncodeParams = ctx->init_encode_params;
2974 
2975  compute_dar(avctx, &dw, &dh);
2976  if (dw != ctx->init_encode_params.darWidth || dh != ctx->init_encode_params.darHeight) {
2977  av_log(avctx, AV_LOG_VERBOSE,
2978  "aspect ratio change (DAR): %d:%d -> %d:%d\n",
2979  ctx->init_encode_params.darWidth,
2980  ctx->init_encode_params.darHeight, dw, dh);
2981 
2982  params.reInitEncodeParams.darHeight = dh;
2983  params.reInitEncodeParams.darWidth = dw;
2984 
2985  needs_reconfig = 1;
2986  reconfig_dar = 1;
2987  }
2988 
2989  if (ctx->rc != NV_ENC_PARAMS_RC_CONSTQP && ctx->support_dyn_bitrate) {
2990  if (avctx->bit_rate > 0 && params.reInitEncodeParams.encodeConfig->rcParams.averageBitRate != avctx->bit_rate) {
2991  av_log(avctx, AV_LOG_VERBOSE,
2992  "avg bitrate change: %d -> %d\n",
2993  params.reInitEncodeParams.encodeConfig->rcParams.averageBitRate,
2994  (uint32_t)avctx->bit_rate);
2995 
2996  params.reInitEncodeParams.encodeConfig->rcParams.averageBitRate = avctx->bit_rate;
2997  reconfig_bitrate = 1;
2998  }
2999 
3000  if (avctx->rc_max_rate > 0 && ctx->encode_config.rcParams.maxBitRate != avctx->rc_max_rate) {
3001  av_log(avctx, AV_LOG_VERBOSE,
3002  "max bitrate change: %d -> %d\n",
3003  params.reInitEncodeParams.encodeConfig->rcParams.maxBitRate,
3004  (uint32_t)avctx->rc_max_rate);
3005 
3006  params.reInitEncodeParams.encodeConfig->rcParams.maxBitRate = avctx->rc_max_rate;
3007  reconfig_bitrate = 1;
3008  }
3009 
3010  if (avctx->rc_buffer_size > 0 && ctx->encode_config.rcParams.vbvBufferSize != avctx->rc_buffer_size) {
3011  av_log(avctx, AV_LOG_VERBOSE,
3012  "vbv buffer size change: %d -> %d\n",
3013  params.reInitEncodeParams.encodeConfig->rcParams.vbvBufferSize,
3014  avctx->rc_buffer_size);
3015 
3016  params.reInitEncodeParams.encodeConfig->rcParams.vbvBufferSize = avctx->rc_buffer_size;
3017  reconfig_bitrate = 1;
3018  }
3019 
3020  if (reconfig_bitrate) {
3021  params.resetEncoder = 1;
3022  params.forceIDR = 1;
3023 
3024  needs_encode_config = 1;
3025  needs_reconfig = 1;
3026  }
3027  }
3028 
3029  if (!needs_encode_config)
3030  params.reInitEncodeParams.encodeConfig = NULL;
3031 
3032  if (needs_reconfig) {
3033  ret = p_nvenc->nvEncReconfigureEncoder(ctx->nvencoder, &params);
3034  if (ret != NV_ENC_SUCCESS) {
3035  nvenc_print_error(avctx, ret, "failed to reconfigure nvenc");
3036  } else {
3037  if (reconfig_dar) {
3038  ctx->init_encode_params.darHeight = dh;
3039  ctx->init_encode_params.darWidth = dw;
3040  }
3041 
3042  if (reconfig_bitrate) {
3043  ctx->encode_config.rcParams.averageBitRate = params.reInitEncodeParams.encodeConfig->rcParams.averageBitRate;
3044  ctx->encode_config.rcParams.maxBitRate = params.reInitEncodeParams.encodeConfig->rcParams.maxBitRate;
3045  ctx->encode_config.rcParams.vbvBufferSize = params.reInitEncodeParams.encodeConfig->rcParams.vbvBufferSize;
3046  }
3047 
3048  }
3049  }
3050 }
3051 
3052 #ifdef NVENC_HAVE_HEVC_AND_AV1_MASTERING_METADATA
3053 static int nvenc_set_mastering_display_data(AVCodecContext *avctx, const AVFrame *frame, NV_ENC_PIC_PARAMS *pic_params,
3054  MASTERING_DISPLAY_INFO *mastering_disp_info, CONTENT_LIGHT_LEVEL *content_light_level)
3055 {
3056  NvencContext *ctx = avctx->priv_data;
3057 
3058  if (ctx->mdm || ctx->cll) {
3059  const AVFrameSideData *sd_mdm = av_frame_get_side_data(frame, AV_FRAME_DATA_MASTERING_DISPLAY_METADATA);
3060  const AVFrameSideData *sd_cll = av_frame_get_side_data(frame, AV_FRAME_DATA_CONTENT_LIGHT_LEVEL);
3061  const int chroma_den = (avctx->codec->id == AV_CODEC_ID_AV1) ? 1 << 16 : 50000;
3062  const int max_luma_den = (avctx->codec->id == AV_CODEC_ID_AV1) ? 1 << 8 : 10000;
3063  const int min_luma_den = (avctx->codec->id == AV_CODEC_ID_AV1) ? 1 << 14 : 10000;
3064 
3065  if (!sd_mdm)
3066  sd_mdm = av_frame_side_data_get(avctx->decoded_side_data,
3067  avctx->nb_decoded_side_data,
3068  AV_FRAME_DATA_MASTERING_DISPLAY_METADATA);
3069  if (!sd_cll)
3070  sd_cll = av_frame_side_data_get(avctx->decoded_side_data,
3071  avctx->nb_decoded_side_data,
3072  AV_FRAME_DATA_CONTENT_LIGHT_LEVEL);
3073 
3074  if (sd_mdm) {
3075  const AVMasteringDisplayMetadata *mdm = (AVMasteringDisplayMetadata *)sd_mdm->data;
3076 
3077  mastering_disp_info->r.x = av_rescale(mdm->display_primaries[0][0].num, chroma_den,
3078  mdm->display_primaries[0][0].den);
3079  mastering_disp_info->r.y = av_rescale(mdm->display_primaries[0][1].num, chroma_den,
3080  mdm->display_primaries[0][1].den);
3081  mastering_disp_info->g.x = av_rescale(mdm->display_primaries[1][0].num, chroma_den,
3082  mdm->display_primaries[1][0].den);
3083  mastering_disp_info->g.y = av_rescale(mdm->display_primaries[1][1].num, chroma_den,
3084  mdm->display_primaries[1][1].den);
3085  mastering_disp_info->b.x = av_rescale(mdm->display_primaries[2][0].num, chroma_den,
3086  mdm->display_primaries[2][0].den);
3087  mastering_disp_info->b.y = av_rescale(mdm->display_primaries[2][1].num, chroma_den,
3088  mdm->display_primaries[2][1].den);
3089  mastering_disp_info->whitePoint.x = av_rescale(mdm->white_point[0].num, chroma_den,
3090  mdm->white_point[0].den);
3091  mastering_disp_info->whitePoint.y = av_rescale(mdm->white_point[1].num, chroma_den,
3092  mdm->white_point[1].den);
3093  mastering_disp_info->maxLuma = av_rescale(mdm->max_luminance.num, max_luma_den,
3094  mdm->max_luminance.den);
3095  mastering_disp_info->minLuma = av_rescale(mdm->min_luminance.num, min_luma_den,
3096  mdm->min_luminance.den);
3097 
3098  if (avctx->codec->id == AV_CODEC_ID_HEVC)
3099  pic_params->codecPicParams.hevcPicParams.pMasteringDisplay = mastering_disp_info;
3100  else if (avctx->codec->id == AV_CODEC_ID_AV1)
3101  pic_params->codecPicParams.av1PicParams.pMasteringDisplay = mastering_disp_info;
3102  else
3103  return AVERROR_BUG;
3104  }
3105  if (sd_cll) {
3106  const AVContentLightMetadata *cll = (AVContentLightMetadata *)sd_cll->data;
3107 
3108  content_light_level->maxContentLightLevel = cll->MaxCLL;
3109  content_light_level->maxPicAverageLightLevel = cll->MaxFALL;
3110 
3111  if (avctx->codec->id == AV_CODEC_ID_HEVC)
3112  pic_params->codecPicParams.hevcPicParams.pMaxCll = content_light_level;
3113  else if (avctx->codec->id == AV_CODEC_ID_AV1)
3114  pic_params->codecPicParams.av1PicParams.pMaxCll = content_light_level;
3115  else
3116  return AVERROR_BUG;
3117  }
3118  }
3119 
3120  return 0;
3121 }
3122 #endif
3123 
3124 static int nvenc_send_frame(AVCodecContext *avctx, const AVFrame *frame)
3125 {
3126  NVENCSTATUS nv_status;
3127  NvencSurface *tmp_out_surf, *in_surf;
3128  int res, res2;
3129  int sei_count = 0;
3130  int i;
3131 #ifdef NVENC_HAVE_HEVC_AND_AV1_MASTERING_METADATA
3132  MASTERING_DISPLAY_INFO mastering_disp_info = { 0 };
3133  CONTENT_LIGHT_LEVEL content_light_level = { 0 };
3134 #endif
3135 #ifdef NVENC_HAVE_MVHEVC
3136  HEVC_3D_REFERENCE_DISPLAY_INFO ref_disp_info = { 0 };
3137 #endif
3138 
3139  NvencContext *ctx = avctx->priv_data;
3140  NvencDynLoadFunctions *dl_fn = &ctx->nvenc_dload_funcs;
3141  NV_ENCODE_API_FUNCTION_LIST *p_nvenc = &dl_fn->nvenc_funcs;
3142 
3143  NV_ENC_PIC_PARAMS pic_params = { 0 };
3144  pic_params.version = NV_ENC_PIC_PARAMS_VER;
3145 
3146  if ((!ctx->cu_context && !ctx->d3d11_device) || !ctx->nvencoder)
3147  return AVERROR(EINVAL);
3148 
3149  if (frame && frame->buf[0]) {
3150  in_surf = get_free_frame(ctx);
3151  if (!in_surf)
3152  return AVERROR(EAGAIN);
3153 
3154  res = nvenc_push_context(avctx);
3155  if (res < 0)
3156  return res;
3157 
3158  reconfig_encoder(avctx, frame);
3159 
3160  res = nvenc_upload_frame(avctx, frame, in_surf);
3161 
3162  res2 = nvenc_pop_context(avctx);
3163  if (res2 < 0)
3164  return res2;
3165 
3166  if (res)
3167  return res;
3168 
3169  pic_params.inputBuffer = in_surf->input_surface;
3170  pic_params.bufferFmt = in_surf->format;
3171  pic_params.inputWidth = in_surf->width;
3172  pic_params.inputHeight = in_surf->height;
3173  pic_params.inputPitch = in_surf->pitch;
3174  pic_params.outputBitstream = in_surf->output_surface;
3175 
3176  if (avctx->flags & AV_CODEC_FLAG_INTERLACED_DCT) {
3177  if (frame->flags & AV_FRAME_FLAG_TOP_FIELD_FIRST)
3178  pic_params.pictureStruct = NV_ENC_PIC_STRUCT_FIELD_TOP_BOTTOM;
3179  else
3180  pic_params.pictureStruct = NV_ENC_PIC_STRUCT_FIELD_BOTTOM_TOP;
3181  } else {
3182  pic_params.pictureStruct = NV_ENC_PIC_STRUCT_FRAME;
3183  }
3184 
3185  if (ctx->forced_idr >= 0 && frame->pict_type == AV_PICTURE_TYPE_I) {
3186  pic_params.encodePicFlags =
3187  ctx->forced_idr ? NV_ENC_PIC_FLAG_FORCEIDR : NV_ENC_PIC_FLAG_FORCEINTRA;
3188  } else {
3189  pic_params.encodePicFlags = 0;
3190  }
3191 
3192  pic_params.frameIdx = ctx->frame_idx_counter++;
3193  pic_params.inputTimeStamp = frame->pts;
3194 
3195  if (ctx->extra_sei) {
3196  res = prepare_sei_data_array(avctx, frame);
3197  if (res < 0)
3198  return res;
3199  sei_count = res;
3200  }
3201 
3202 #ifdef NVENC_HAVE_HEVC_AND_AV1_MASTERING_METADATA
3203  res = nvenc_set_mastering_display_data(avctx, frame, &pic_params, &mastering_disp_info, &content_light_level);
3204  if (res < 0)
3205  return res;
3206 #endif
3207 
3208 #ifdef NVENC_HAVE_MVHEVC
3209  if (ctx->multiview) {
3210  const AVFrameSideData *sd_tdrdi = av_frame_get_side_data(frame, AV_FRAME_DATA_3D_REFERENCE_DISPLAYS);
3211  const AVFrameSideData *sd_view_id = av_frame_get_side_data(frame, AV_FRAME_DATA_VIEW_ID);
3212 
3213  if (sd_view_id)
3214  ctx->next_view_id = *(int*)sd_view_id->data;
3215 
3216  pic_params.codecPicParams.hevcPicParams.viewId = ctx->next_view_id;
3217 
3218  if (sd_tdrdi) {
3219  AV3DReferenceDisplaysInfo *tdrdi = (AV3DReferenceDisplaysInfo*)sd_tdrdi->data;
3220 
3221  ref_disp_info.refViewingDistanceFlag = tdrdi->ref_viewing_distance_flag;
3222  ref_disp_info.precRefViewingDist = tdrdi->prec_ref_viewing_dist;
3223  ref_disp_info.precRefDisplayWidth = tdrdi->prec_ref_display_width;
3224 
3225  ref_disp_info.numRefDisplaysMinus1 = tdrdi->num_ref_displays - 1;
3226 
3227  for (i = 0; i < tdrdi->num_ref_displays &&
3228  i < FF_ARRAY_ELEMS(ref_disp_info.leftViewId); i++) {
3229  const AV3DReferenceDisplay *display = av_tdrdi_get_display(tdrdi, i);
3230  ref_disp_info.leftViewId[i] = display->left_view_id;
3231  ref_disp_info.rightViewId[i] = display->right_view_id;
3232  ref_disp_info.exponentRefDisplayWidth[i] = display->exponent_ref_display_width;
3233  ref_disp_info.mantissaRefDisplayWidth[i] = display->mantissa_ref_display_width;
3234  ref_disp_info.exponentRefViewingDistance[i] = display->exponent_ref_viewing_distance;
3235  ref_disp_info.mantissaRefViewingDistance[i] = display->mantissa_ref_viewing_distance;
3236  ref_disp_info.additionalShiftPresentFlag[i] = display->additional_shift_present_flag;
3237  ref_disp_info.numSampleShiftPlus512[i] = display->num_sample_shift + 512;
3238  }
3239 
3240  pic_params.codecPicParams.hevcPicParams.p3DReferenceDisplayInfo = &ref_disp_info;
3241  ctx->display_sei_sent = 1;
3242  } else if (!ctx->display_sei_sent) {
3243  ref_disp_info.precRefDisplayWidth = 31;
3244  ref_disp_info.leftViewId[0] = 0;
3245  ref_disp_info.rightViewId[0] = 1;
3246 
3247  pic_params.codecPicParams.hevcPicParams.p3DReferenceDisplayInfo = &ref_disp_info;
3248  ctx->display_sei_sent = 1;
3249  }
3250 
3251  ctx->next_view_id = !ctx->next_view_id;
3252  }
3253 #endif
3254 
3255  res = nvenc_store_frame_data(avctx, &pic_params, frame);
3256  if (res < 0)
3257  return res;
3258 
3259  nvenc_codec_specific_pic_params(avctx, frame, &pic_params, ctx->sei_data, sei_count);
3260  } else {
3261  pic_params.encodePicFlags = NV_ENC_PIC_FLAG_EOS;
3262  }
3263 
3264  res = nvenc_push_context(avctx);
3265  if (res < 0)
3266  return res;
3267 
3268  nv_status = p_nvenc->nvEncEncodePicture(ctx->nvencoder, &pic_params);
3269 
3270  for (i = 0; i < sei_count; i++)
3271  av_freep(&(ctx->sei_data[i].payload));
3272 
3273  res = nvenc_pop_context(avctx);
3274  if (res < 0)
3275  return res;
3276 
3277  if (nv_status != NV_ENC_SUCCESS &&
3278  nv_status != NV_ENC_ERR_NEED_MORE_INPUT)
3279  return nvenc_print_error(avctx, nv_status, "EncodePicture failed!");
3280 
3281  if (frame && frame->buf[0]) {
3282  av_fifo_write(ctx->output_surface_queue, &in_surf, 1);
3283 
3284  if (avctx->codec_descriptor->props & AV_CODEC_PROP_REORDER)
3285  timestamp_queue_enqueue(ctx->timestamp_list, frame->pts);
3286  }
3287 
3288  /* all the pending buffers are now ready for output */
3289  if (nv_status == NV_ENC_SUCCESS) {
3290  while (av_fifo_read(ctx->output_surface_queue, &tmp_out_surf, 1) >= 0)
3291  av_fifo_write(ctx->output_surface_ready_queue, &tmp_out_surf, 1);
3292  }
3293 
3294  return 0;
3295 }
3296 
3297 int ff_nvenc_receive_packet(AVCodecContext *avctx, AVPacket *pkt)
3298 {
3299  NvencSurface *tmp_out_surf;
3300  int res, res2;
3301 
3302  NvencContext *ctx = avctx->priv_data;
3303 
3304  AVFrame *frame = ctx->frame;
3305 
3306  if ((!ctx->cu_context && !ctx->d3d11_device) || !ctx->nvencoder)
3307  return AVERROR(EINVAL);
3308 
3309  if (!frame->buf[0]) {
3310  res = ff_encode_get_frame(avctx, frame);
3311  if (res < 0 && res != AVERROR_EOF)
3312  return res;
3313  }
3314 
3315  res = nvenc_send_frame(avctx, frame);
3316  if (res < 0) {
3317  if (res != AVERROR(EAGAIN))
3318  return res;
3319  } else
3320  av_frame_unref(frame);
3321 
3322  if (output_ready(avctx, avctx->internal->draining)) {
3323  av_fifo_read(ctx->output_surface_ready_queue, &tmp_out_surf, 1);
3324 
3325  res = nvenc_push_context(avctx);
3326  if (res < 0)
3327  return res;
3328 
3329  res = process_output_surface(avctx, pkt, tmp_out_surf);
3330 
3331  res2 = nvenc_pop_context(avctx);
3332  if (res2 < 0)
3333  return res2;
3334 
3335  if (res)
3336  return res;
3337 
3338  av_fifo_write(ctx->unused_surface_queue, &tmp_out_surf, 1);
3339  } else if (avctx->internal->draining) {
3340  return AVERROR_EOF;
3341  } else {
3342  return AVERROR(EAGAIN);
3343  }
3344 
3345  return 0;
3346 }
3347 
3348 av_cold void ff_nvenc_encode_flush(AVCodecContext *avctx)
3349 {
3350  NvencContext *ctx = avctx->priv_data;
3351 
3352  nvenc_send_frame(avctx, NULL);
3353  av_fifo_reset2(ctx->timestamp_list);
3354  ctx->output_frame_num = 0;
3355  ctx->initial_delay_time = 0;
3356 }
error
static void error(const char *err)
Definition: target_bsf_fuzzer.c:32
flags
const SwsFlags flags[]
Definition: swscale.c:72
NVENC_LOSSLESS
@ NVENC_LOSSLESS
Definition: nvenc.h:194
AVHWDeviceContext::hwctx
void * hwctx
The format-specific data, allocated and freed by libavutil along with this context.
Definition: hwcontext.h:88
ff_alloc_a53_sei
int ff_alloc_a53_sei(const AVFrame *frame, size_t prefix_len, void **data, size_t *sei_size)
Check AVFrame for A53 side data and allocate and fill SEI message with A53 info.
Definition: atsc_a53.c:26
AV_LOG_WARNING
#define AV_LOG_WARNING
Something somehow does not look correct.
Definition: log.h:216
PRESET_ALIAS
#define PRESET_ALIAS(alias, name,...)
Definition: nvenc.c:205
AV_PIX_FMT_CUDA
@ AV_PIX_FMT_CUDA
HW acceleration through CUDA.
Definition: pixfmt.h:260
AV3DReferenceDisplay::num_sample_shift
int16_t num_sample_shift
The recommended additional horizontal shift for a stereo pair corresponding to the n-th reference bas...
Definition: tdrdi.h:141
AVMasteringDisplayMetadata::max_luminance
AVRational max_luminance
Max luminance of mastering display (cd/m^2).
Definition: mastering_display_metadata.h:57
AVPixelFormat
AVPixelFormat
Pixel format.
Definition: pixfmt.h:71
name
it s the only field you need to keep assuming you have a context There is some magic you don t need to care about around this just let it vf default minimum maximum flags name is the option name
Definition: writing_filters.txt:88
GUIDTuple::guid
const GUID guid
Definition: nvenc.c:201
level
uint8_t level
Definition: svq3.c:208
av_clip
#define av_clip
Definition: common.h:100
AVERROR
Filter the word “frame” indicates either a video frame or a group of audio as stored in an AVFrame structure Format for each input and each output the list of supported formats For video that means pixel format For audio that means channel sample they are references to shared objects When the negotiation mechanism computes the intersection of the formats supported at each end of a all references to both lists are replaced with a reference to the intersection And when a single format is eventually chosen for a link amongst the remaining all references to the list are updated That means that if a filter requires that its input and output have the same format amongst a supported all it has to do is use a reference to the same list of formats query_formats can leave some formats unset and return AVERROR(EAGAIN) to cause the negotiation mechanism toagain later. That can be used by filters with complex requirements to use the format negotiated on one link to set the formats supported on another. Frame references ownership and permissions
AVCodecContext::colorspace
enum AVColorSpace colorspace
YUV colorspace type.
Definition: avcodec.h:671
NVENC_RGB_MODE_DISABLED
@ NVENC_RGB_MODE_DISABLED
Definition: nvenc.h:207
AVCodecContext::decoded_side_data
AVFrameSideData ** decoded_side_data
Array containing static side data, such as HDR10 CLL / MDCV structures.
Definition: avcodec.h:1942
av_frame_get_side_data
AVFrameSideData * av_frame_get_side_data(const AVFrame *frame, enum AVFrameSideDataType type)
Definition: frame.c:659
AV_PIX_FMT_BGR32
#define AV_PIX_FMT_BGR32
Definition: pixfmt.h:513
GUIDTuple
Definition: nvenc.c:200
GUIDTuple::flags
int flags
Definition: nvenc.c:202
av_pix_fmt_desc_get
const AVPixFmtDescriptor * av_pix_fmt_desc_get(enum AVPixelFormat pix_fmt)
Definition: pixdesc.c:3456
AVERROR_EOF
#define AVERROR_EOF
End of file.
Definition: error.h:57
AVBufferRef::data
uint8_t * data
The data buffer.
Definition: buffer.h:90
timecode_internal.h
AV_FRAME_DATA_A53_CC
@ AV_FRAME_DATA_A53_CC
ATSC A53 Part 4 Closed Captions.
Definition: frame.h:59
AV_PROFILE_H264_MAIN
#define AV_PROFILE_H264_MAIN
Definition: defs.h:112
nvenc_push_context
static int nvenc_push_context(AVCodecContext *avctx)
Definition: nvenc.c:394
AVMasteringDisplayMetadata::display_primaries
AVRational display_primaries[3][2]
CIE 1931 xy chromaticity coords of color primaries (r, g, b order).
Definition: mastering_display_metadata.h:42
AVHWFramesContext::format
enum AVPixelFormat format
The pixel format identifying the underlying HW surface type.
Definition: hwcontext.h:200
AVPictureType
AVPictureType
Definition: avutil.h:276
output_ready
static int output_ready(AVCodecContext *avctx, int flush)
Definition: nvenc.c:2836
NvencContext
Definition: nvenc.h:212
AV3DReferenceDisplaysInfo::prec_ref_viewing_dist
uint8_t prec_ref_viewing_dist
The exponent of the maximum allowable truncation error for {exponent,mantissa}_ref_viewing_distance a...
Definition: tdrdi.h:72
AVCodecContext::codec_descriptor
const struct AVCodecDescriptor * codec_descriptor
AVCodecDescriptor.
Definition: avcodec.h:1722
int64_t
long long int64_t
Definition: coverity.c:34
av_tdrdi_get_display
static av_always_inline AV3DReferenceDisplay * av_tdrdi_get_display(AV3DReferenceDisplaysInfo *tdrdi, unsigned int idx)
Definition: tdrdi.h:145
AV_PIX_FMT_YUV444P10MSB
#define AV_PIX_FMT_YUV444P10MSB
Definition: pixfmt.h:554
AV_FRAME_DATA_S12M_TIMECODE
@ AV_FRAME_DATA_S12M_TIMECODE
Timecode which conforms to SMPTE ST 12-1.
Definition: frame.h:152
AV_PROFILE_HEVC_MAIN
#define AV_PROFILE_HEVC_MAIN
Definition: defs.h:159
NvencSurface::in_ref
AVFrame * in_ref
Definition: nvenc.h:117
av_frame_free
void av_frame_free(AVFrame **frame)
Free the frame and any dynamically allocated objects in it, e.g.
Definition: frame.c:64
AVContentLightMetadata::MaxCLL
unsigned MaxCLL
Max content light level (cd/m^2).
Definition: mastering_display_metadata.h:111
nvenc_store_frame_data
static int nvenc_store_frame_data(AVCodecContext *avctx, NV_ENC_PIC_PARAMS *pic_params, const AVFrame *frame)
Definition: nvenc.c:2689
av_fifo_peek
int av_fifo_peek(const AVFifo *f, void *buf, size_t nb_elems, size_t offset)
Read data from a FIFO without modifying FIFO state.
Definition: fifo.c:255
AV3DReferenceDisplay
Data structure for single deference display information.
Definition: tdrdi.h:100
AVFrame
This structure describes decoded (raw) audio or video data.
Definition: frame.h:459
pixdesc.h
AVCodecContext::color_trc
enum AVColorTransferCharacteristic color_trc
Color Transfer Characteristic.
Definition: avcodec.h:664
nvenc_set_timestamp
static int nvenc_set_timestamp(AVCodecContext *avctx, NV_ENC_LOCK_BITSTREAM *params, AVPacket *pkt)
Definition: nvenc.c:2632
AVCOL_RANGE_JPEG
@ AVCOL_RANGE_JPEG
Full range content.
Definition: pixfmt.h:777
internal.h
AVPacket::data
uint8_t * data
Definition: packet.h:595
encode.h
AVCodecContext::b_quant_offset
float b_quant_offset
qscale offset between IP and B-frames
Definition: avcodec.h:797
NvencFrameData
Definition: nvenc.h:127
reconfig_encoder
static void reconfig_encoder(AVCodecContext *avctx, const AVFrame *frame)
Definition: nvenc.c:2960
AV_LOG_VERBOSE
#define AV_LOG_VERBOSE
Detailed information.
Definition: log.h:226
AVCOL_SPC_RGB
@ AVCOL_SPC_RGB
order of coefficients is actually GBR, also IEC 61966-2-1 (sRGB), YZX and ST 428-1
Definition: pixfmt.h:701
timestamp_queue_peek
static int64_t timestamp_queue_peek(AVFifo *queue, size_t index)
Definition: nvenc.c:2624
ff_nvenc_pix_fmts
enum AVPixelFormat ff_nvenc_pix_fmts[]
Definition: nvenc.c:59
set_constqp
static av_cold void set_constqp(AVCodecContext *avctx)
Definition: nvenc.c:885
NvencSurface
Definition: nvenc.h:114
AVPacket::duration
int64_t duration
Duration of this packet in AVStream->time_base units, 0 if unknown.
Definition: packet.h:613
mathematics.h
FFMAX
#define FFMAX(a, b)
Definition: macros.h:47
av_buffer_ref
AVBufferRef * av_buffer_ref(const AVBufferRef *buf)
Create a new reference to an AVBuffer.
Definition: buffer.c:103
nvenc_print_error
static int nvenc_print_error(AVCodecContext *avctx, NVENCSTATUS err, const char *error_string)
Definition: nvenc.c:180
BD
#define BD
AVERROR_UNKNOWN
#define AVERROR_UNKNOWN
Unknown error, typically from an external library.
Definition: error.h:73
AVCodecContext::qmax
int qmax
maximum quantizer
Definition: avcodec.h:1259
nverr
NVENCSTATUS nverr
Definition: nvenc.c:133
NONE
#define NONE
Definition: vf_drawvg.c:262
set_lossless
static av_cold void set_lossless(AVCodecContext *avctx)
Definition: nvenc.c:1000
PRESET
#define PRESET(name,...)
Definition: nvenc.c:208
AV_PKT_FLAG_KEY
#define AV_PKT_FLAG_KEY
The packet contains a keyframe.
Definition: packet.h:650
dummy
static int dummy
Definition: ffplay.c:3751
ff_nvenc_encode_flush
av_cold void ff_nvenc_encode_flush(AVCodecContext *avctx)
Definition: nvenc.c:3348
AV_STEREO3D_UNSPEC
@ AV_STEREO3D_UNSPEC
Video is stereoscopic but the packing is unspecified.
Definition: stereo3d.h:143
AV_CODEC_FLAG_GLOBAL_HEADER
#define AV_CODEC_FLAG_GLOBAL_HEADER
Place global headers in extradata instead of every keyframe.
Definition: avcodec.h:318
ff_timecode_set_smpte
void ff_timecode_set_smpte(unsigned *drop, unsigned *hh, unsigned *mm, unsigned *ss, unsigned *ff, AVRational rate, uint32_t tcsmpte, int prevent_df, int skip_field)
Convert SMPTE 12M binary representation to sei info.
Definition: timecode_internal.c:33
nvenc.h
AV_FRAME_FLAG_TOP_FIELD_FIRST
#define AV_FRAME_FLAG_TOP_FIELD_FIRST
A flag to mark frames where the top field is displayed first if the content is interlaced.
Definition: frame.h:687
av_memdup
void * av_memdup(const void *p, size_t size)
Duplicate a buffer with av_malloc().
Definition: mem.c:304
AV_HWDEVICE_TYPE_CUDA
@ AV_HWDEVICE_TYPE_CUDA
Definition: hwcontext.h:30
AVContentLightMetadata
Content light level needed by to transmit HDR over HDMI (CTA-861.3).
Definition: mastering_display_metadata.h:107
compute_dar
static void compute_dar(AVCodecContext *avctx, int *dw, int *dh)
Definition: nvenc.c:1801
AV3DReferenceDisplaysInfo
This structure describes information about the reference display width(s) and reference viewing dista...
Definition: tdrdi.h:53
AVCodecContext::framerate
AVRational framerate
Definition: avcodec.h:563
AVCOL_SPC_BT470BG
@ AVCOL_SPC_BT470BG
also ITU-R BT601-6 625 / ITU-R BT1358 625 / ITU-R BT1700 625 PAL & SECAM / IEC 61966-2-4 xvYCC601
Definition: pixfmt.h:706
nvenc_upload_frame
static int nvenc_upload_frame(AVCodecContext *avctx, const AVFrame *frame, NvencSurface *nvenc_frame)
Definition: nvenc.c:2452
NVENC_TWO_PASSES
@ NVENC_TWO_PASSES
Definition: nvenc.h:196
NvencDynLoadFunctions::nvenc_device_count
int nvenc_device_count
Definition: nvenc.h:141
AV_CODEC_FLAG_COPY_OPAQUE
#define AV_CODEC_FLAG_COPY_OPAQUE
Definition: avcodec.h:279
AVCodecContext::i_quant_factor
float i_quant_factor
qscale factor between P- and I-frames If > 0 then the last P-frame quantizer will be used (q = lastp_...
Definition: avcodec.h:806
set_vbr
static av_cold void set_vbr(AVCodecContext *avctx)
Definition: nvenc.c:923
nvenc_map_error
static int nvenc_map_error(NVENCSTATUS err, const char **desc)
Definition: nvenc.c:165
AVCodecContext::codec
const struct AVCodec * codec
Definition: avcodec.h:452
AVPacket::opaque_ref
AVBufferRef * opaque_ref
AVBufferRef for free use by the API user.
Definition: packet.h:631
nvenc_check_cap
static int nvenc_check_cap(AVCodecContext *avctx, NV_ENC_CAPS cap)
Definition: nvenc.c:479
presets
static const Preset presets[]
Definition: vf_pseudocolor.c:286
fail
#define fail()
Definition: checkasm.h:225
av_fifo_write
int av_fifo_write(AVFifo *f, const void *buf, size_t nb_elems)
Write data into a FIFO.
Definition: fifo.c:188
AV_STEREO3D_2D
@ AV_STEREO3D_2D
Video is not stereoscopic (and metadata has to be there).
Definition: stereo3d.h:52
NVENC_LOWLATENCY
@ NVENC_LOWLATENCY
Definition: nvenc.h:193
NvencSurface::format
NV_ENC_BUFFER_FORMAT format
Definition: nvenc.h:124
nvenc_setup_rate_control
static av_cold int nvenc_setup_rate_control(AVCodecContext *avctx)
Definition: nvenc.c:1092
sei.h
AVCodecContext::refs
int refs
number of reference frames
Definition: avcodec.h:701
AV_HWDEVICE_TYPE_D3D11VA
@ AV_HWDEVICE_TYPE_D3D11VA
Definition: hwcontext.h:35
nvenc_map_preset
static void nvenc_map_preset(NvencContext *ctx)
Definition: nvenc.c:210
AVCodecContext::flags
int flags
AV_CODEC_FLAG_*.
Definition: avcodec.h:500
val
static double val(void *priv, double ch)
Definition: aeval.c:77
nvenc_copy_frame
static int nvenc_copy_frame(AVCodecContext *avctx, NvencSurface *nv_surface, NV_ENC_LOCK_INPUT_BUFFER *lock_buffer_params, const AVFrame *frame)
Definition: nvenc.c:2334
AVERROR_BUFFER_TOO_SMALL
#define AVERROR_BUFFER_TOO_SMALL
Buffer too small.
Definition: error.h:53
hwcontext_cuda.h
av_image_fill_pointers
int av_image_fill_pointers(uint8_t *data[4], enum AVPixelFormat pix_fmt, int height, uint8_t *ptr, const int linesizes[4])
Fill plane data pointers for an image with pixel format pix_fmt and height height.
Definition: imgutils.c:145
ss
#define ss(width, name, subs,...)
Definition: cbs_vp9.c:202
IS_GBRP
#define IS_GBRP(pix_fmt)
Definition: nvenc.c:128
ff_encode_add_stats_side_data
int ff_encode_add_stats_side_data(AVPacket *pkt, int quality, const int64_t error[], int error_count, enum AVPictureType pict_type)
Definition: encode.c:947
AVCUDADeviceContext::cuda_ctx
CUcontext cuda_ctx
Definition: hwcontext_cuda.h:43
av_reduce
int av_reduce(int *dst_num, int *dst_den, int64_t num, int64_t den, int64_t max)
Reduce a fraction.
Definition: rational.c:35
nvenc_print_driver_requirement
static void nvenc_print_driver_requirement(AVCodecContext *avctx, int level)
Definition: nvenc.c:264
AVRational::num
int num
Numerator.
Definition: rational.h:59
AV_CODEC_FLAG_INTERLACED_DCT
#define AV_CODEC_FLAG_INTERLACED_DCT
Use interlaced DCT.
Definition: avcodec.h:310
nvenc_check_capabilities
static int nvenc_check_capabilities(AVCodecContext *avctx)
Definition: nvenc.c:496
AVHWDeviceContext
This struct aggregates all the (hardware/vendor-specific) "high-level" state, i.e.
Definition: hwcontext.h:63
av_frame_alloc
AVFrame * av_frame_alloc(void)
Allocate an AVFrame and set its fields to default values.
Definition: frame.c:52
AVCodecContext::color_primaries
enum AVColorPrimaries color_primaries
Chromaticity coordinates of the source primaries.
Definition: avcodec.h:657
AV_STEREO3D_FRAMESEQUENCE
@ AV_STEREO3D_FRAMESEQUENCE
Views are alternated temporally.
Definition: stereo3d.h:89
AV_LOG_ERROR
#define AV_LOG_ERROR
Something went wrong and cannot losslessly be recovered.
Definition: log.h:210
AVFrameSideData::size
size_t size
Definition: frame.h:317
FF_ARRAY_ELEMS
#define FF_ARRAY_ELEMS(a)
Definition: sinewin_tablegen.c:29
av_cold
#define av_cold
Definition: attributes.h:119
to_nv_color_pri
#define to_nv_color_pri(n)
Definition: nvenc.c:346
av_fifo_read
int av_fifo_read(AVFifo *f, void *buf, size_t nb_elems)
Read data from a FIFO.
Definition: fifo.c:240
P2
#define P2
Definition: cavsdsp.c:36
AV_PIX_FMT_YUVJ422P
@ AV_PIX_FMT_YUVJ422P
planar YUV 4:2:2, 16bpp, full scale (JPEG), deprecated in favor of AV_PIX_FMT_YUV422P and setting col...
Definition: pixfmt.h:86
AVCodecContext::extradata_size
int extradata_size
Definition: avcodec.h:527
AVCodecContext::has_b_frames
int has_b_frames
Size of the frame reordering buffer in the decoder.
Definition: avcodec.h:709
ff_nvenc_encode_init
av_cold int ff_nvenc_encode_init(AVCodecContext *avctx)
Definition: nvenc.c:2271
av_fast_realloc
void * av_fast_realloc(void *ptr, unsigned int *size, size_t min_size)
Reallocate the given buffer if it is not large enough, otherwise do nothing.
Definition: mem.c:497
stereo3d.h
AVMasteringDisplayMetadata::white_point
AVRational white_point[2]
CIE 1931 xy chromaticity coords of white point.
Definition: mastering_display_metadata.h:47
AVCodecContext::global_quality
int global_quality
Global quality for codecs which cannot change it per frame.
Definition: avcodec.h:1235
AVD3D11VADeviceContext::device
ID3D11Device * device
Device used for texture creation and access.
Definition: hwcontext_d3d11va.h:56
AV_PIX_FMT_YUV444P16
#define AV_PIX_FMT_YUV444P16
Definition: pixfmt.h:552
AVFormatContext::flags
int flags
Flags modifying the (de)muxer behaviour.
Definition: avformat.h:1434
AVCodecContext::nb_decoded_side_data
int nb_decoded_side_data
Definition: avcodec.h:1943
AV_PIX_FMT_0BGR32
#define AV_PIX_FMT_0BGR32
Definition: pixfmt.h:516
pix_fmt
static enum AVPixelFormat pix_fmt
Definition: demux_decode.c:41
NvencDynLoadFunctions
Definition: nvenc.h:135
AV_PROFILE_H264_HIGH_10
#define AV_PROFILE_H264_HIGH_10
Definition: defs.h:115
NV_ENC_H264_PROFILE_HIGH
@ NV_ENC_H264_PROFILE_HIGH
Definition: nvenc.h:171
ctx
static AVFormatContext * ctx
Definition: movenc.c:49
SEI_TYPE_USER_DATA_REGISTERED_ITU_T_T35
@ SEI_TYPE_USER_DATA_REGISTERED_ITU_T_T35
Definition: sei.h:34
av_rescale_q
int64_t av_rescale_q(int64_t a, AVRational bq, AVRational cq)
Rescale a 64-bit integer by 2 rational numbers.
Definition: mathematics.c:142
AV_FRAME_DATA_3D_REFERENCE_DISPLAYS
@ AV_FRAME_DATA_3D_REFERENCE_DISPLAYS
This side data contains information about the reference display width(s) and reference viewing distan...
Definition: frame.h:256
nvenc_setup_extradata
static av_cold int nvenc_setup_extradata(AVCodecContext *avctx)
Definition: nvenc.c:2152
timestamp_queue_enqueue
static void timestamp_queue_enqueue(AVFifo *queue, int64_t timestamp)
Definition: nvenc.c:2610
P1
#define P1
Definition: cavsdsp.c:37
AV_PIX_FMT_YUV420P
@ AV_PIX_FMT_YUV420P
planar YUV 4:2:0, 12bpp, (1 Cr & Cb sample per 2x2 Y samples)
Definition: pixfmt.h:73
AVCodecContext::rc_max_rate
int64_t rc_max_rate
maximum bitrate
Definition: avcodec.h:1288
timestamp_queue_dequeue
static int64_t timestamp_queue_dequeue(AVFifo *queue)
Definition: nvenc.c:2615
av_mallocz
#define av_mallocz(s)
Definition: tableprint_vlc.h:31
AVPacket::opaque
void * opaque
for some private data of the user
Definition: packet.h:620
NvencDynLoadFunctions::nvenc_dl
NvencFunctions * nvenc_dl
Definition: nvenc.h:138
AVCPBProperties
This structure describes the bitrate properties of an encoded bitstream.
Definition: defs.h:282
av_fallthrough
#define av_fallthrough
Definition: attributes.h:67
AV_CODEC_ID_H264
@ AV_CODEC_ID_H264
Definition: codec_id.h:79
LIST_DEVICES
@ LIST_DEVICES
Definition: nvenc.h:202
NvencSurface::pitch
int pitch
Definition: nvenc.h:121
tmp
static uint8_t tmp[40]
Definition: aes_ctr.c:52
AV_PIX_FMT_YUVJ444P
@ AV_PIX_FMT_YUVJ444P
planar YUV 4:4:4, 24bpp, full scale (JPEG), deprecated in favor of AV_PIX_FMT_YUV444P and setting col...
Definition: pixfmt.h:87
AV_PROFILE_H264_HIGH_422
#define AV_PROFILE_H264_HIGH_422
Definition: defs.h:118
AVCodecContext::codec_id
enum AVCodecID codec_id
Definition: avcodec.h:453
NvencSurface::input_surface
NV_ENC_INPUT_PTR input_surface
Definition: nvenc.h:116
AVCodecDescriptor::props
int props
Codec properties, a combination of AV_CODEC_PROP_* flags.
Definition: codec_desc.h:54
if
if(ret)
Definition: filter_design.txt:179
AVCodecContext::rc_buffer_size
int rc_buffer_size
decoder bitstream buffer size
Definition: avcodec.h:1273
NVENC_CAP
#define NVENC_CAP
Definition: nvenc.c:49
AV_PIX_FMT_GBRP16
#define AV_PIX_FMT_GBRP16
Definition: pixfmt.h:561
IS_10BIT
#define IS_10BIT(pix_fmt)
Definition: nvenc.c:98
AV3DReferenceDisplaysInfo::ref_viewing_distance_flag
uint8_t ref_viewing_distance_flag
A flag to indicate the presence of reference viewing distance.
Definition: tdrdi.h:65
fabs
static __device__ float fabs(float a)
Definition: cuda_runtime.h:182
NULL
#define NULL
Definition: coverity.c:32
AVHWFramesContext::sw_format
enum AVPixelFormat sw_format
The pixel format identifying the actual data layout of the hardware frames.
Definition: hwcontext.h:213
IS_YUV422
#define IS_YUV422(pix_fmt)
Definition: nvenc.c:124
NvencSurface::reg_idx
int reg_idx
Definition: nvenc.h:118
AVCodecContext::color_range
enum AVColorRange color_range
MPEG vs JPEG YUV range.
Definition: avcodec.h:681
av_buffer_unref
void av_buffer_unref(AVBufferRef **buf)
Free a given reference and automatically free the buffer if there are no more references to it.
Definition: buffer.c:139
SEI_TYPE_TIME_CODE
@ SEI_TYPE_TIME_CODE
Definition: sei.h:95
AV_CODEC_ID_AV1
@ AV_CODEC_ID_AV1
Definition: codec_id.h:284
AVRational
Rational number (pair of numerator and denominator).
Definition: rational.h:58
NVENC_ONE_PASS
@ NVENC_ONE_PASS
Definition: nvenc.h:195
AVCodecContext::internal
struct AVCodecInternal * internal
Private context used for internal data.
Definition: avcodec.h:478
AV_PIX_FMT_YUVJ420P
@ AV_PIX_FMT_YUVJ420P
planar YUV 4:2:0, 12bpp, full scale (JPEG), deprecated in favor of AV_PIX_FMT_YUV420P and setting col...
Definition: pixfmt.h:85
AVCodecContext::bit_rate
int64_t bit_rate
the average bitrate
Definition: avcodec.h:493
ff_nvenc_encode_close
av_cold int ff_nvenc_encode_close(AVCodecContext *avctx)
Definition: nvenc.c:2186
FrameData::duration
int64_t duration
Definition: librav1e.c:60
AV_PICTURE_TYPE_I
@ AV_PICTURE_TYPE_I
Intra.
Definition: avutil.h:278
AV3DReferenceDisplay::exponent_ref_display_width
uint8_t exponent_ref_display_width
The exponent part of the reference display width of the n-th reference display.
Definition: tdrdi.h:114
P3
#define P3
Definition: dsp_template.c:820
av_fifo_can_read
size_t av_fifo_can_read(const AVFifo *f)
Definition: fifo.c:87
flush
void(* flush)(AVBSFContext *ctx)
Definition: dts2pts.c:553
FrameData::frame_opaque
void * frame_opaque
Definition: librav1e.c:62
NvencDynLoadFunctions::cuda_dl
CudaFunctions * cuda_dl
Definition: nvenc.h:137
AV_FRAME_DATA_MASTERING_DISPLAY_METADATA
@ AV_FRAME_DATA_MASTERING_DISPLAY_METADATA
Mastering display metadata associated with a video frame.
Definition: frame.h:120
nvenc_setup_h264_config
static av_cold int nvenc_setup_h264_config(AVCodecContext *avctx)
Definition: nvenc.c:1278
AV3DReferenceDisplaysInfo::prec_ref_display_width
uint8_t prec_ref_display_width
The exponent of the maximum allowable truncation error for {exponent,mantissa}_ref_display_width as g...
Definition: tdrdi.h:58
ANY_DEVICE
@ ANY_DEVICE
Definition: nvenc.h:203
AVPixFmtDescriptor::flags
uint64_t flags
Combination of AV_PIX_FMT_FLAG_...
Definition: pixdesc.h:94
AV_PROFILE_HEVC_MAIN_10
#define AV_PROFILE_HEVC_MAIN_10
Definition: defs.h:160
AV_PROFILE_HEVC_REXT
#define AV_PROFILE_HEVC_REXT
Definition: defs.h:162
index
int index
Definition: gxfenc.c:90
AV_FRAME_DATA_SEI_UNREGISTERED
@ AV_FRAME_DATA_SEI_UNREGISTERED
User data unregistered metadata associated with a video frame.
Definition: frame.h:178
AVCodecContext::time_base
AVRational time_base
This is the fundamental unit of time (in seconds) in terms of which frame timestamps are represented.
Definition: avcodec.h:547
av_fifo_reset2
void av_fifo_reset2(AVFifo *f)
Definition: fifo.c:280
AV_PIX_FMT_X2BGR10
#define AV_PIX_FMT_X2BGR10
Definition: pixfmt.h:614
AVCUDADeviceContext::stream
CUstream stream
Definition: hwcontext_cuda.h:44
desc
const char * desc
Definition: nvenc.c:135
nvenc_pop_context
static int nvenc_pop_context(AVCodecContext *avctx)
Definition: nvenc.c:405
HW_CONFIG_ENCODER_DEVICE
#define HW_CONFIG_ENCODER_DEVICE(format, device_type_)
Definition: hwconfig.h:95
AVFifo
Definition: fifo.c:35
AVCodecContext::gop_size
int gop_size
the number of pictures in a group of pictures, or 0 for intra_only
Definition: avcodec.h:1021
height
#define height
Definition: dsp.h:89
av_frame_ref
int av_frame_ref(AVFrame *dst, const AVFrame *src)
Set up a new reference to the data described by the source frame.
Definition: frame.c:278
nvenc_check_codec_support
static int nvenc_check_codec_support(AVCodecContext *avctx)
Definition: nvenc.c:443
AV_PIX_FMT_FLAG_RGB
#define AV_PIX_FMT_FLAG_RGB
The pixel format contains RGB-like data (as opposed to YUV/grayscale).
Definition: pixdesc.h:136
AV_CODEC_PROP_REORDER
#define AV_CODEC_PROP_REORDER
Codec supports frame reordering.
Definition: codec_desc.h:92
ff_nvenc_hw_configs
const AVCodecHWConfigInternal *const ff_nvenc_hw_configs[]
Definition: nvenc.c:88
i
#define i(width, name, range_min, range_max)
Definition: cbs_h264.c:63
MAX_REGISTERED_FRAMES
#define MAX_REGISTERED_FRAMES
Definition: nvenc.h:41
ff_alloc_timecode_sei
int ff_alloc_timecode_sei(const AVFrame *frame, AVRational rate, size_t prefix_len, void **data, size_t *sei_size)
Check AVFrame for S12M timecode side data and allocate and fill TC SEI message with timecode info.
Definition: utils.c:982
P6
#define P6
Definition: filter_template.c:407
for
for(k=2;k<=8;++k)
Definition: h264pred_template.c:424
nvenc_alloc_surface
static av_cold int nvenc_alloc_surface(AVCodecContext *avctx, int idx)
Definition: nvenc.c:2050
AV_NOPTS_VALUE
#define AV_NOPTS_VALUE
Undefined timestamp value.
Definition: avutil.h:247
AVFrameSideData::data
uint8_t * data
Definition: frame.h:316
nvenc_check_device
static av_cold int nvenc_check_device(AVCodecContext *avctx, int idx)
Definition: nvenc.c:694
nvenc_register_frame
static int nvenc_register_frame(AVCodecContext *avctx, const AVFrame *frame)
Definition: nvenc.c:2398
AVCodecHWConfigInternal
Definition: hwconfig.h:25
frame_data
FrameData * frame_data(AVFrame *frame)
Get our axiliary frame data attached to the frame, allocating it if needed.
Definition: ffmpeg.c:477
AV_PIX_FMT_NV16
@ AV_PIX_FMT_NV16
interleaved chroma YUV 4:2:2, 16bpp, (1 Cr & Cb sample per 2x1 Y samples)
Definition: pixfmt.h:198
ff_nvenc_receive_packet
int ff_nvenc_receive_packet(AVCodecContext *avctx, AVPacket *pkt)
Definition: nvenc.c:3297
AVPacket::dts
int64_t dts
Decompression timestamp in AVStream->time_base units; the time at which the packet is decompressed.
Definition: packet.h:594
AV_PIX_FMT_RGB32
#define AV_PIX_FMT_RGB32
Definition: pixfmt.h:511
nvenc_override_rate_control
static void nvenc_override_rate_control(AVCodecContext *avctx)
Definition: nvenc.c:1014
AVERROR_EXTERNAL
#define AVERROR_EXTERNAL
Generic error in an external library.
Definition: error.h:59
AVPacket::flags
int flags
A combination of AV_PKT_FLAG values.
Definition: packet.h:601
AV_PIX_FMT_D3D11
@ AV_PIX_FMT_D3D11
Hardware surfaces for Direct3D11.
Definition: pixfmt.h:336
AV_PIX_FMT_P216
#define AV_PIX_FMT_P216
Definition: pixfmt.h:620
FrameData::frame_opaque_ref
AVBufferRef * frame_opaque_ref
Definition: librav1e.c:63
xf
#define xf(width, name, var, range_min, range_max, subs,...)
Definition: cbs_av1.c:622
AVCPBProperties::avg_bitrate
int64_t avg_bitrate
Average bitrate of the stream, in bits per second.
Definition: defs.h:297
AV_PIX_FMT_P210
#define AV_PIX_FMT_P210
Definition: pixfmt.h:616
NV_ENC_H264_PROFILE_BASELINE
@ NV_ENC_H264_PROFILE_BASELINE
Definition: nvenc.h:169
get_free_frame
static NvencSurface * get_free_frame(NvencContext *ctx)
Definition: nvenc.c:2323
NV_ENC_HEVC_PROFILE_MAIN
@ NV_ENC_HEVC_PROFILE_MAIN
Definition: nvenc.h:182
AV_LOG_INFO
#define AV_LOG_INFO
Standard information.
Definition: log.h:221
AVCodecContext::b_quant_factor
float b_quant_factor
qscale factor between IP and B-frames If > 0 then the last P-frame quantizer will be used (q= lastp_q...
Definition: avcodec.h:790
AV_FRAME_DATA_VIEW_ID
@ AV_FRAME_DATA_VIEW_ID
This side data must be associated with a video frame.
Definition: frame.h:245
AVCodec::id
enum AVCodecID id
Definition: codec.h:186
nvenc_open_session
static av_cold int nvenc_open_session(AVCodecContext *avctx)
Definition: nvenc.c:417
HW_CONFIG_ENCODER_FRAMES
#define HW_CONFIG_ENCODER_FRAMES(format, device_type_)
Definition: hwconfig.h:98
AV_FRAME_DATA_CONTENT_LIGHT_LEVEL
@ AV_FRAME_DATA_CONTENT_LIGHT_LEVEL
Content light level (based on CTA-861.3).
Definition: frame.h:137
AV3DReferenceDisplay::right_view_id
uint16_t right_view_id
The ViewId of the left view of a stereo pair corresponding to the n-th reference display.
Definition: tdrdi.h:109
av_malloc
#define av_malloc(s)
Definition: ops_asmgen.c:44
AVPacket::pts
int64_t pts
Presentation timestamp in AVStream->time_base units; the time at which the decompressed packet will b...
Definition: packet.h:588
FAST
@ FAST
Definition: vf_guided.c:32
AVCodecContext::extradata
uint8_t * extradata
Out-of-band global headers that may be used by some codecs.
Definition: avcodec.h:526
process_output_surface
static int process_output_surface(AVCodecContext *avctx, AVPacket *pkt, NvencSurface *tmpoutsurf)
Definition: nvenc.c:2736
nvenc_load_libraries
static av_cold int nvenc_load_libraries(AVCodecContext *avctx)
Definition: nvenc.c:350
nvenc_recalc_surfaces
static av_cold int nvenc_recalc_surfaces(AVCodecContext *avctx)
Definition: nvenc.c:1049
AVD3D11VADeviceContext
This struct is allocated as AVHWDeviceContext.hwctx.
Definition: hwcontext_d3d11va.h:45
IS_RGB
#define IS_RGB(pix_fmt)
Definition: nvenc.c:109
AVCPBProperties::max_bitrate
int64_t max_bitrate
Maximum bitrate of the stream, in bits per second.
Definition: defs.h:287
AV_CODEC_ID_HEVC
@ AV_CODEC_ID_HEVC
Definition: codec_id.h:228
nvenc_errors
static const struct @226 nvenc_errors[]
prepare_sei_data_array
static int prepare_sei_data_array(AVCodecContext *avctx, const AVFrame *frame)
Definition: nvenc.c:2848
AV_FRAME_DATA_STEREO3D
@ AV_FRAME_DATA_STEREO3D
Stereoscopic 3d metadata.
Definition: frame.h:64
AV1_METADATA_TYPE_TIMECODE
@ AV1_METADATA_TYPE_TIMECODE
Definition: av1.h:48
FFMIN
#define FFMIN(a, b)
Definition: macros.h:49
av_frame_unref
void av_frame_unref(AVFrame *frame)
Unreference all the buffers referenced by frame and reset the frame fields.
Definition: frame.c:496
AV_PIX_FMT_X2RGB10
#define AV_PIX_FMT_X2RGB10
Definition: pixfmt.h:613
AV3DReferenceDisplay::mantissa_ref_display_width
uint8_t mantissa_ref_display_width
The mantissa part of the reference display width of the n-th reference display.
Definition: tdrdi.h:119
AVCodecContext::hw_device_ctx
AVBufferRef * hw_device_ctx
A reference to the AVHWDeviceContext describing the device which will be used by a hardware encoder/d...
Definition: avcodec.h:1493
AVMasteringDisplayMetadata
Mastering display metadata capable of representing the color volume of the display used to master the...
Definition: mastering_display_metadata.h:38
IS_YUV444
#define IS_YUV444(pix_fmt)
Definition: nvenc.c:116
IS_CBR
#define IS_CBR(rc)
Definition: nvenc.c:52
av_rescale
int64_t av_rescale(int64_t a, int64_t b, int64_t c)
Rescale a 64-bit integer with rounding to nearest.
Definition: mathematics.c:129
AVCodecContext::height
int height
Definition: avcodec.h:604
AVCodecContext::pix_fmt
enum AVPixelFormat pix_fmt
Pixel format, see AV_PIX_FMT_xxx.
Definition: avcodec.h:643
CHECK_CU
#define CHECK_CU(x)
Definition: nvenc.c:47
nvenc_map_buffer_format
static NV_ENC_BUFFER_FORMAT nvenc_map_buffer_format(enum AVPixelFormat pix_fmt)
Definition: nvenc.c:2010
av_calloc
void * av_calloc(size_t nmemb, size_t size)
Definition: mem.c:264
AV_PIX_FMT_P016
#define AV_PIX_FMT_P016
Definition: pixfmt.h:604
AVCodecContext::hw_frames_ctx
AVBufferRef * hw_frames_ctx
A reference to the AVHWFramesContext describing the input (for encoding) or output (decoding) frames.
Definition: avcodec.h:1471
NvencSurface::width
int width
Definition: nvenc.h:119
AVHWFramesContext
This struct describes a set or pool of "hardware" frames (i.e.
Definition: hwcontext.h:118
AVCUDADeviceContext
This struct is allocated as AVHWDeviceContext.hwctx.
Definition: hwcontext_cuda.h:42
AV_PROFILE_H264_HIGH_444_PREDICTIVE
#define AV_PROFILE_H264_HIGH_444_PREDICTIVE
Definition: defs.h:122
ret
ret
Definition: filter_design.txt:187
AV_LOG_FATAL
#define AV_LOG_FATAL
Something went wrong and recovery is not possible.
Definition: log.h:204
AVHWDeviceContext::type
enum AVHWDeviceType type
This field identifies the underlying API used for hardware access.
Definition: hwcontext.h:75
nvenc_setup_encoder
static av_cold int nvenc_setup_encoder(AVCodecContext *avctx)
Definition: nvenc.c:1834
AV_PIX_FMT_NV12
@ AV_PIX_FMT_NV12
planar YUV 4:2:0, 12bpp, 1 plane for Y and 1 plane for the UV components, which are interleaved (firs...
Definition: pixfmt.h:96
FFSWAP
#define FFSWAP(type, a, b)
Definition: macros.h:52
frame
these buffered frames must be flushed immediately if a new input produces new the filter must not call request_frame to get more It must just process the frame or queue it The task of requesting more frames is left to the filter s request_frame method or the application If a filter has several the filter must be ready for frames arriving randomly on any input any filter with several inputs will most likely require some kind of queuing mechanism It is perfectly acceptable to have a limited queue and to drop frames when the inputs are too unbalanced request_frame For filters that do not use the this method is called when a frame is wanted on an output For a it should directly call filter_frame on the corresponding output For a if there are queued frames already one of these frames should be pushed If the filter should request a frame on one of its repeatedly until at least one frame has been pushed Return or at least make progress towards producing a frame
Definition: filter_design.txt:265
averr
int averr
Definition: nvenc.c:134
AV_PIX_FMT_0RGB32
#define AV_PIX_FMT_0RGB32
Definition: pixfmt.h:515
AVHWFramesContext::device_ctx
AVHWDeviceContext * device_ctx
The parent AVHWDeviceContext.
Definition: hwcontext.h:137
AVCPBProperties::buffer_size
int64_t buffer_size
The size of the buffer to which the ratecontrol is applied, in bits.
Definition: defs.h:303
cuda_check.h
atsc_a53.h
AVStereo3D::type
enum AVStereo3DType type
How views are packed within the video.
Definition: stereo3d.h:207
AV_PROFILE_H264_BASELINE
#define AV_PROFILE_H264_BASELINE
Definition: defs.h:110
AV3DReferenceDisplay::mantissa_ref_viewing_distance
uint8_t mantissa_ref_viewing_distance
The mantissa part of the reference viewing distance of the n-th reference display.
Definition: tdrdi.h:129
av_fifo_alloc2
AVFifo * av_fifo_alloc2(size_t nb_elems, size_t elem_size, unsigned int flags)
Allocate and initialize an AVFifo with a given element size.
Definition: fifo.c:47
AV_INPUT_BUFFER_PADDING_SIZE
#define AV_INPUT_BUFFER_PADDING_SIZE
Definition: defs.h:40
AVCodecContext
main external API structure.
Definition: avcodec.h:443
AV_PROFILE_H264_HIGH
#define AV_PROFILE_H264_HIGH
Definition: defs.h:114
AV1_METADATA_TYPE_ITUT_T35
@ AV1_METADATA_TYPE_ITUT_T35
Definition: av1.h:47
AV_PICTURE_TYPE_B
@ AV_PICTURE_TYPE_B
Bi-dir predicted.
Definition: avutil.h:280
ff_get_encode_buffer
int ff_get_encode_buffer(AVCodecContext *avctx, AVPacket *avpkt, int64_t size, int flags)
Get a buffer for a packet.
Definition: encode.c:105
NvencSurface::height
int height
Definition: nvenc.h:120
SEI_TYPE_USER_DATA_UNREGISTERED
@ SEI_TYPE_USER_DATA_UNREGISTERED
Definition: sei.h:35
av_image_copy2
static void av_image_copy2(uint8_t *const dst_data[4], const int dst_linesizes[4], uint8_t *const src_data[4], const int src_linesizes[4], enum AVPixelFormat pix_fmt, int width, int height)
Wrapper around av_image_copy() to workaround the limitation that the conversion from uint8_t * const ...
Definition: imgutils.h:184
AVCodecContext::qmin
int qmin
minimum quantizer
Definition: avcodec.h:1252
AVRational::den
int den
Denominator.
Definition: rational.h:60
AV_PIX_FMT_NONE
@ AV_PIX_FMT_NONE
Definition: pixfmt.h:72
AVCodecContext::profile
int profile
profile
Definition: avcodec.h:1636
nvenc_setup_surfaces
static av_cold int nvenc_setup_surfaces(AVCodecContext *avctx)
Definition: nvenc.c:2106
AV3DReferenceDisplay::additional_shift_present_flag
uint8_t additional_shift_present_flag
An array of flags to indicates that the information about additional horizontal shift of the left and...
Definition: tdrdi.h:135
AVCodecContext::i_quant_offset
float i_quant_offset
qscale offset between P and I-frames
Definition: avcodec.h:813
AVFrameSideData::type
enum AVFrameSideDataType type
Definition: frame.h:315
NvencSurface::output_surface
NV_ENC_OUTPUT_PTR output_surface
Definition: nvenc.h:123
AV_PROFILE_HEVC_MULTIVIEW_MAIN
#define AV_PROFILE_HEVC_MULTIVIEW_MAIN
Definition: defs.h:163
nvenc_find_free_reg_resource
static int nvenc_find_free_reg_resource(AVCodecContext *avctx)
Definition: nvenc.c:2364
nvenc_codec_specific_pic_params
static void nvenc_codec_specific_pic_params(AVCodecContext *avctx, const AVFrame *frame, NV_ENC_PIC_PARAMS *params, NV_ENC_SEI_PAYLOAD *sei_data, int sei_count)
Definition: nvenc.c:2559
AVMasteringDisplayMetadata::min_luminance
AVRational min_luminance
Min luminance of mastering display (cd/m^2).
Definition: mastering_display_metadata.h:52
AV_PIX_FMT_YUV444P
@ AV_PIX_FMT_YUV444P
planar YUV 4:4:4, 24bpp, (1 Cr & Cb sample per 1x1 Y samples)
Definition: pixfmt.h:78
P7
#define P7
Definition: filter_template.c:406
AV_PIX_FMT_P010
#define AV_PIX_FMT_P010
Definition: pixfmt.h:602
AVCodecInternal::draining
int draining
decoding: AVERROR_EOF has been returned from ff_decode_get_packet(); must not be used by decoders tha...
Definition: internal.h:139
AV_PIX_FMT_GBRP
@ AV_PIX_FMT_GBRP
planar GBR 4:4:4 24bpp
Definition: pixfmt.h:165
AV3DReferenceDisplaysInfo::num_ref_displays
uint8_t num_ref_displays
The number of reference displays that are signalled in this struct.
Definition: tdrdi.h:78
NvencDynLoadFunctions::nvenc_funcs
NV_ENCODE_API_FUNCTION_LIST nvenc_funcs
Definition: nvenc.h:140
AV_PICTURE_TYPE_P
@ AV_PICTURE_TYPE_P
Predicted.
Definition: avutil.h:279
mem.h
AVCodecContext::max_b_frames
int max_b_frames
maximum number of B-frames between non-B-frames Note: The output will be delayed by max_b_frames+1 re...
Definition: avcodec.h:781
ff_encode_get_frame
int ff_encode_get_frame(AVCodecContext *avctx, AVFrame *frame)
Called by encoders to get the next frame for encoding.
Definition: encode.c:217
AV3DReferenceDisplay::exponent_ref_viewing_distance
uint8_t exponent_ref_viewing_distance
The exponent part of the reference viewing distance of the n-th reference display.
Definition: tdrdi.h:124
mastering_display_metadata.h
AVFrameSideData
Structure to hold side data for an AVFrame.
Definition: frame.h:314
AVPixFmtDescriptor
Descriptor that unambiguously describes how the bits of a pixel are stored in the up to 4 data planes...
Definition: pixdesc.h:69
P4
#define P4
Definition: filter_template.c:409
av_free
#define av_free(p)
Definition: tableprint_vlc.h:34
AVCodecContext::slices
int slices
Number of slices.
Definition: avcodec.h:1037
to_nv_color_matrix
#define to_nv_color_matrix(n)
Definition: nvenc.c:345
DEFAULT
#define DEFAULT
Definition: avdct.c:30
AVContentLightMetadata::MaxFALL
unsigned MaxFALL
Max average light level per frame (cd/m^2).
Definition: mastering_display_metadata.h:116
AVPacket
This structure stores compressed data.
Definition: packet.h:572
to_nv_color_trc
#define to_nv_color_trc(n)
Definition: nvenc.c:347
AVCodecContext::priv_data
void * priv_data
Definition: avcodec.h:470
NV_ENC_HEVC_PROFILE_REXT
@ NV_ENC_HEVC_PROFILE_REXT
Definition: nvenc.h:184
av_freep
#define av_freep(p)
Definition: tableprint_vlc.h:35
NV_ENC_H264_PROFILE_HIGH_444P
@ NV_ENC_H264_PROFILE_HIGH_444P
Definition: nvenc.h:178
AV_PICTURE_TYPE_BI
@ AV_PICTURE_TYPE_BI
BI type.
Definition: avutil.h:284
nvenc_setup_device
static av_cold int nvenc_setup_device(AVCodecContext *avctx)
Definition: nvenc.c:769
P5
#define P5
Definition: filter_template.c:408
av_frame_side_data_get
static const AVFrameSideData * av_frame_side_data_get(AVFrameSideData *const *sd, const int nb_sd, enum AVFrameSideDataType type)
Wrapper around av_frame_side_data_get_c() to workaround the limitation that for any type T the conver...
Definition: frame.h:1183
AVCodecContext::width
int width
picture width / height.
Definition: avcodec.h:604
imgutils.h
hwcontext.h
AVERROR_BUG
#define AVERROR_BUG
Internal bug, also see AVERROR_BUG2.
Definition: error.h:52
av_log
#define av_log(a,...)
Definition: tableprint_vlc.h:27
av_fifo_freep2
void av_fifo_freep2(AVFifo **f)
Free an AVFifo and reset pointer to NULL.
Definition: fifo.c:286
AVERROR_EXIT
#define AVERROR_EXIT
Immediate exit was requested; the called function should not be restarted.
Definition: error.h:58
AV_PIX_FMT_GBRP10MSB
#define AV_PIX_FMT_GBRP10MSB
Definition: pixfmt.h:568
ff_encode_add_cpb_side_data
AVCPBProperties * ff_encode_add_cpb_side_data(AVCodecContext *avctx)
Add a CPB properties side data to an encoding context.
Definition: encode.c:916
AVStereo3D
Stereo 3D type: this structure describes how two videos are packed within a single video surface,...
Definition: stereo3d.h:203
pkt
static AVPacket * pkt
Definition: demux_decode.c:55
nvenc_setup_codec_config
static av_cold int nvenc_setup_codec_config(AVCodecContext *avctx)
Definition: nvenc.c:1784
width
#define width
Definition: dsp.h:89
FF_QP2LAMBDA
#define FF_QP2LAMBDA
factor to convert from H.263 QP to lambda
Definition: avutil.h:226
NV_ENC_HEVC_PROFILE_MAIN_10
@ NV_ENC_HEVC_PROFILE_MAIN_10
Definition: nvenc.h:183
AV3DReferenceDisplay::left_view_id
uint16_t left_view_id
The ViewId of the left view of a stereo pair corresponding to the n-th reference display.
Definition: tdrdi.h:104
AV_PROFILE_AV1_MAIN
#define AV_PROFILE_AV1_MAIN
Definition: defs.h:169
codec_desc.h
AVCodecContext::sample_aspect_ratio
AVRational sample_aspect_ratio
sample aspect ratio (0 if unknown) That is the width of a pixel divided by the height of the pixel.
Definition: avcodec.h:628
nvenc_setup_hevc_config
static av_cold int nvenc_setup_hevc_config(AVCodecContext *avctx)
Definition: nvenc.c:1474
NVENC_DEPRECATED_PRESET
@ NVENC_DEPRECATED_PRESET
Definition: nvenc.h:198
RC_MODE_DEPRECATED
#define RC_MODE_DEPRECATED
Definition: nvenc.h:42
tdrdi.h
nvenc_send_frame
static int nvenc_send_frame(AVCodecContext *avctx, const AVFrame *frame)
Definition: nvenc.c:3124
av_get_pix_fmt_name
const char * av_get_pix_fmt_name(enum AVPixelFormat pix_fmt)
Return the short name for a pixel format, NULL in case pix_fmt is unknown.
Definition: pixdesc.c:3376
NV_ENC_H264_PROFILE_MAIN
@ NV_ENC_H264_PROFILE_MAIN
Definition: nvenc.h:170
nvenc_retrieve_frame_data
static int nvenc_retrieve_frame_data(AVCodecContext *avctx, NV_ENC_LOCK_BITSTREAM *lock_params, AVPacket *pkt)
Definition: nvenc.c:2715
Generated on Fri May 22 2026 19:22:35 for FFmpeg by   doxygen 1.8.17