Home
last modified time | relevance | path

Searched refs:CHECK_CU (Results 1 – 11 of 11) sorted by relevance

/third_party/ffmpeg/libavutil/
Dhwcontext_cuda.c53 #define CHECK_CU(x) FF_CUDA_CHECK_DL(device_ctx, cu, x) macro
89 CHECK_CU(cu->cuCtxPushCurrent(hwctx->cuda_ctx)); in cuda_buffer_free()
91 CHECK_CU(cu->cuMemFree((CUdeviceptr)data)); in cuda_buffer_free()
93 CHECK_CU(cu->cuCtxPopCurrent(&dummy)); in cuda_buffer_free()
108 err = CHECK_CU(cu->cuCtxPushCurrent(hwctx->cuda_ctx)); in cuda_pool_alloc()
112 err = CHECK_CU(cu->cuMemAlloc(&data, size)); in cuda_pool_alloc()
118 CHECK_CU(cu->cuMemFree(data)); in cuda_pool_alloc()
123 CHECK_CU(cu->cuCtxPopCurrent(&dummy)); in cuda_pool_alloc()
145 err = CHECK_CU(cu->cuDeviceGetAttribute(&priv->tex_alignment, in cuda_frames_init()
236 ret = CHECK_CU(cu->cuCtxPushCurrent(hwctx->cuda_ctx)); in cuda_transfer_data()
[all …]
Dhwcontext_vulkan.c41 #define CHECK_CU(x) FF_CUDA_CHECK_DL(cuda_cu, cu, x) macro
1239 int ret = CHECK_CU(cu->cuDeviceGetUuid((CUuuid *)&dev_select.uuid, in vulkan_device_derive()
1376 CHECK_CU(cu->cuDestroyExternalSemaphore(internal->cu_sem[i])); in vulkan_free_internal()
1378 CHECK_CU(cu->cuMipmappedArrayDestroy(internal->cu_mma[i])); in vulkan_free_internal()
1380 CHECK_CU(cu->cuDestroyExternalMemory(internal->ext_mem[i])); in vulkan_free_internal()
2401 ret = CHECK_CU(cu->cuImportExternalMemory(&dst_int->ext_mem[i], &ext_desc)); in vulkan_export_to_cuda()
2407 ret = CHECK_CU(cu->cuExternalMemoryGetMappedMipmappedArray(&dst_int->cu_mma[i], in vulkan_export_to_cuda()
2415 ret = CHECK_CU(cu->cuMipmappedArrayGetLevel(&dst_int->cu_array[i], in vulkan_export_to_cuda()
2431 ret = CHECK_CU(cu->cuImportExternalSemaphore(&dst_int->cu_sem[i], in vulkan_export_to_cuda()
2465 ret = CHECK_CU(cu->cuCtxPushCurrent(cuda_dev->cuda_ctx)); in vulkan_transfer_data_from_cuda()
[all …]
/third_party/ffmpeg/libavfilter/
Dvf_yadif_cuda.c51 #define CHECK_CU(x) FF_CUDA_CHECK_DL(ctx, s->hwctx->internal->cuda_dl, x) macro
91 ret = CHECK_CU(cu->cuTexObjectCreate(&tex_prev, &res_desc, &tex_desc, NULL)); in call_kernel()
96 ret = CHECK_CU(cu->cuTexObjectCreate(&tex_cur, &res_desc, &tex_desc, NULL)); in call_kernel()
101 ret = CHECK_CU(cu->cuTexObjectCreate(&tex_next, &res_desc, &tex_desc, NULL)); in call_kernel()
105 ret = CHECK_CU(cu->cuLaunchKernel(func, in call_kernel()
112 CHECK_CU(cu->cuTexObjectDestroy(tex_prev)); in call_kernel()
114 CHECK_CU(cu->cuTexObjectDestroy(tex_cur)); in call_kernel()
116 CHECK_CU(cu->cuTexObjectDestroy(tex_next)); in call_kernel()
130 ret = CHECK_CU(cu->cuCtxPushCurrent(s->cu_ctx)); in filter()
184 CHECK_CU(cu->cuCtxPopCurrent(&dummy)); in filter()
[all …]
Dvf_thumbnail_cuda.c32 #define CHECK_CU(x) FF_CUDA_CHECK_DL(ctx, s->hwctx->internal->cuda_dl, x) macro
183 ret = CHECK_CU(cu->cuTexObjectCreate(&tex, &res_desc, &tex_desc, NULL)); in thumbnail_kernel()
187 ret = CHECK_CU(cu->cuLaunchKernel(func, in thumbnail_kernel()
192 CHECK_CU(cu->cuTexObjectDestroy(tex)); in thumbnail_kernel()
262 ret = CHECK_CU(cu->cuCtxPushCurrent(s->hwctx->cuda_ctx)); in filter_frame()
266 CHECK_CU(cu->cuMemsetD8Async(s->data, 0, HIST_SIZE * sizeof(int), s->cu_stream)); in filter_frame()
279 ret = CHECK_CU(cu->cuMemcpy2DAsync(&cpy, s->cu_stream)); in filter_frame()
291 CHECK_CU(cu->cuCtxPopCurrent(&dummy)); in filter_frame()
310 CHECK_CU(cu->cuMemFree(s->data)); in uninit()
315 CHECK_CU(cu->cuModuleUnload(s->cu_module)); in uninit()
[all …]
Dvf_overlay_cuda.c38 #define CHECK_CU(x) FF_CUDA_CHECK_DL(ctx, ctx->hwctx->internal->cuda_dl, x) macro
131 return CHECK_CU(cu->cuLaunchKernel( in overlay_cuda_call_kernel()
175 ret = CHECK_CU(cu->cuCtxPushCurrent(cuda_ctx)); in overlay_cuda_blend()
224 CHECK_CU(cu->cuCtxPopCurrent(&dummy)); in overlay_cuda_blend()
228 CHECK_CU(cu->cuCtxPopCurrent(&dummy)); in overlay_cuda_blend()
256 CHECK_CU(cu->cuCtxPushCurrent(ctx->cu_ctx)); in overlay_cuda_uninit()
257 CHECK_CU(cu->cuModuleUnload(ctx->cu_module)); in overlay_cuda_uninit()
258 CHECK_CU(cu->cuCtxPopCurrent(&dummy)); in overlay_cuda_uninit()
366 err = CHECK_CU(cu->cuCtxPushCurrent(cuda_ctx)); in overlay_cuda_config_output()
371 err = CHECK_CU(cu->cuModuleLoadData(&ctx->cu_module, vf_overlay_cuda_ptx)); in overlay_cuda_config_output()
[all …]
Dvf_scale_cuda.c59 #define CHECK_CU(x) FF_CUDA_CHECK_DL(ctx, s->hwctx->internal->cuda_dl, x) macro
142 CHECK_CU(cu->cuCtxPushCurrent(s->hwctx->cuda_ctx)); in cudascale_uninit()
143 CHECK_CU(cu->cuModuleUnload(s->cu_module)); in cudascale_uninit()
145 CHECK_CU(cu->cuCtxPopCurrent(&dummy)); in cudascale_uninit()
318 ret = CHECK_CU(cu->cuCtxPushCurrent(cuda_ctx)); in cudascale_config_props()
322 ret = CHECK_CU(cu->cuModuleLoadData(&s->cu_module, scaler_ptx)); in cudascale_config_props()
327 CHECK_CU(cu->cuModuleGetFunction(&s->cu_func_uchar, s->cu_module, buf)); in cudascale_config_props()
332 CHECK_CU(cu->cuModuleGetFunction(&s->cu_func_uchar2, s->cu_module, buf)); in cudascale_config_props()
337 CHECK_CU(cu->cuModuleGetFunction(&s->cu_func_uchar4, s->cu_module, buf)); in cudascale_config_props()
342 CHECK_CU(cu->cuModuleGetFunction(&s->cu_func_ushort, s->cu_module, buf)); in cudascale_config_props()
[all …]
Dvf_transpose_npp.c36 #define CHECK_CU(x) FF_CUDA_CHECK_DL(ctx, device_hwctx->internal->cuda_dl, x) macro
415 ret = CHECK_CU(device_hwctx->internal->cuda_dl->cuCtxPushCurrent(device_hwctx->cuda_ctx)); in npptranspose_filter_frame()
421 CHECK_CU(device_hwctx->internal->cuda_dl->cuCtxPopCurrent(&dummy)); in npptranspose_filter_frame()
Dvf_scale_npp.c43 #define CHECK_CU(x) FF_CUDA_CHECK_DL(ctx, device_hwctx->internal->cuda_dl, x) macro
525 ret = CHECK_CU(device_hwctx->internal->cuda_dl->cuCtxPushCurrent(device_hwctx->cuda_ctx)); in nppscale_filter_frame()
531 CHECK_CU(device_hwctx->internal->cuda_dl->cuCtxPopCurrent(&dummy)); in nppscale_filter_frame()
/third_party/ffmpeg/libavcodec/
Dnvdec.c60 #define CHECK_CU(x) FF_CUDA_CHECK_DL(logctx, decoder->cudl, x) macro
123 ret = CHECK_CU(decoder->cvdl->cuvidGetDecoderCaps(&caps)); in nvdec_test_capabilities()
168 CHECK_CU(decoder->cudl->cuCtxPushCurrent(decoder->cuda_ctx)); in nvdec_decoder_free()
169 CHECK_CU(decoder->cvdl->cuvidDestroyDecoder(decoder->decoder)); in nvdec_decoder_free()
170 CHECK_CU(decoder->cudl->cuCtxPopCurrent(&dummy)); in nvdec_decoder_free()
219 ret = CHECK_CU(decoder->cudl->cuCtxPushCurrent(decoder->cuda_ctx)); in nvdec_decoder_create()
225 CHECK_CU(decoder->cudl->cuCtxPopCurrent(&dummy)); in nvdec_decoder_create()
229 ret = CHECK_CU(decoder->cvdl->cuvidCreateDecoder(&decoder->decoder, params)); in nvdec_decoder_create()
231 CHECK_CU(decoder->cudl->cuCtxPopCurrent(&dummy)); in nvdec_decoder_create()
465 ret = CHECK_CU(decoder->cudl->cuCtxPushCurrent(decoder->cuda_ctx)); in nvdec_unmap_mapped_frame()
[all …]
Dcuviddec.c108 #define CHECK_CU(x) FF_CUDA_CHECK_DL(avctx, ctx->cudl, x) macro
257 ctx->internal_error = CHECK_CU(ctx->cvdl->cuvidDestroyDecoder(ctx->cudecoder)); in cuvid_handle_video_sequence()
313 ctx->internal_error = CHECK_CU(ctx->cvdl->cuvidCreateDecoder(&ctx->cudecoder, &cuinfo)); in cuvid_handle_video_sequence()
341 ctx->internal_error = CHECK_CU(ctx->cvdl->cuvidDecodePicture(ctx->cudecoder, picparams)); in cuvid_handle_picture_decode()
402 ret = CHECK_CU(ctx->cudl->cuCtxPushCurrent(cuda_ctx)); in cuvid_decode_packet()
425 ret = CHECK_CU(ctx->cvdl->cuvidParseVideoData(ctx->cuparser, &cupkt)); in cuvid_decode_packet()
438 eret = CHECK_CU(ctx->cudl->cuCtxPopCurrent(&dummy)); in cuvid_decode_packet()
481 ret = CHECK_CU(ctx->cudl->cuCtxPushCurrent(cuda_ctx)); in cuvid_output_frame()
500 …ret = CHECK_CU(ctx->cvdl->cuvidMapVideoFrame(ctx->cudecoder, parsed_frame.dispinfo.picture_index, … in cuvid_output_frame()
533 ret = CHECK_CU(ctx->cudl->cuMemcpy2DAsync(&cpy, device_hwctx->stream)); in cuvid_output_frame()
[all …]
Dnvenc.c39 #define CHECK_CU(x) FF_CUDA_CHECK_DL(avctx, dl_fn->cuda_dl, x) macro
313 return CHECK_CU(dl_fn->cuda_dl->cuCtxPushCurrent(ctx->cu_context)); in nvenc_push_context()
325 return CHECK_CU(dl_fn->cuda_dl->cuCtxPopCurrent(&dummy)); in nvenc_pop_context()
537 ret = CHECK_CU(dl_fn->cuda_dl->cuDeviceGet(&cu_device, idx)); in nvenc_check_device()
541 ret = CHECK_CU(dl_fn->cuda_dl->cuDeviceGetName(name, sizeof(name), cu_device)); in nvenc_check_device()
545 ret = CHECK_CU(dl_fn->cuda_dl->cuDeviceComputeCapability(&major, &minor, cu_device)); in nvenc_check_device()
558 ret = CHECK_CU(dl_fn->cuda_dl->cuCtxCreate(&ctx->cu_context_internal, 0, cu_device)); in nvenc_check_device()
592 CHECK_CU(dl_fn->cuda_dl->cuCtxDestroy(ctx->cu_context_internal)); in nvenc_check_device()
676 if (CHECK_CU(dl_fn->cuda_dl->cuInit(0)) < 0) in nvenc_setup_device()
679 if (CHECK_CU(dl_fn->cuda_dl->cuDeviceGetCount(&nb_devices)) < 0) in nvenc_setup_device()
[all …]