Home
last modified time | relevance | path

Searched refs:coding (Results 1 – 25 of 118) sorted by relevance

12345

/rockchip-linux_mpp/osal/driver/
H A Dvcodec_service.c138 const char *mpp_get_platform_dev_name(MppCtxType type, MppCodingType coding, RK_U32 platform) in mpp_get_platform_dev_name() argument
143 (coding == MPP_VIDEO_CodingAVC || in mpp_get_platform_dev_name()
144 coding == MPP_VIDEO_CodingHEVC || in mpp_get_platform_dev_name()
145 coding == MPP_VIDEO_CodingAVS2 || in mpp_get_platform_dev_name()
146 coding == MPP_VIDEO_CodingVP9)) { in mpp_get_platform_dev_name()
149 (coding == MPP_VIDEO_CodingHEVC)) { in mpp_get_platform_dev_name()
152 (coding == MPP_VIDEO_CodingAVS)) { in mpp_get_platform_dev_name()
155 (coding == MPP_VIDEO_CodingAVC)) { in mpp_get_platform_dev_name()
158 (coding == MPP_VIDEO_CodingHEVC)) { in mpp_get_platform_dev_name()
171 const char *mpp_get_vcodec_dev_name(MppCtxType type, MppCodingType coding) in mpp_get_vcodec_dev_name() argument
[all …]
/rockchip-linux_mpp/mpp/hal/rkdec/avsd/
H A Dhal_avsd_api.c38 static MPP_RET init_hard_platform(AvsdHalCtx_t *p_hal, MppCodingType coding) in init_hard_platform() argument
45 if (coding == MPP_VIDEO_CodingAVSPLUS) { in init_hard_platform()
48 coding, vcodec_type, HAVE_AVSDEC); in init_hard_platform()
54 coding, vcodec_type, hw_flag); in init_hard_platform()
57 if ((coding == MPP_VIDEO_CodingAVSPLUS) && in init_hard_platform()
68 } else if ((coding == MPP_VIDEO_CodingAVS) && in init_hard_platform()
79 } else if ((coding == MPP_VIDEO_CodingAVS) && in init_hard_platform()
94 p_hal->coding = coding; in init_hard_platform()
95 AVSD_HAL_DBG(AVSD_DBG_HARD_MODE, "hw_spt %08x, coding %d\n", vcodec_type, coding); in init_hard_platform()
167 FUN_CHECK(ret = init_hard_platform(p_hal, cfg->coding)); in hal_avsd_init()
[all …]
/rockchip-linux_mpp/mpp/base/
H A Dmpp_2str.c33 const char *strof_coding_type(MppCodingType coding) in strof_coding_type() argument
60 if (coding >= MPP_VIDEO_CodingUnused && coding <= MPP_VIDEO_CodingVP9) in strof_coding_type()
61 return coding_type_str0[coding]; in strof_coding_type()
62 else if (coding >= MPP_VIDEO_CodingVC1 && coding <= MPP_VIDEO_CodingAV1) in strof_coding_type()
63 return coding_type_str1[coding - MPP_VIDEO_CodingVC1]; in strof_coding_type()
96 const char *strof_profle(MppCodingType coding, RK_U32 profile) in strof_profle() argument
118 switch (coding) { in strof_profle()
H A Dmpp_dec_cfg.c29 ENTRY(prefix, u32, rk_u32, coding, FLAG_INCR, base, coding) \
64 cfg->base.coding = MPP_VIDEO_CodingUnused; in mpp_dec_cfg_set_default()
/rockchip-linux_mpp/mpp/hal/common/
H A Dhal_info.c28 MppCodingType coding; member
36 MPP_RET hal_info_init(HalInfo *ctx, MppCtxType type, MppCodingType coding) in hal_info_init() argument
49 impl->coding = coding; in hal_info_init()
194 MppCodingType coding = *((MppCodingType *)val); in hal_info_to_string() local
196 mpp_assert(coding == info->coding); in hal_info_to_string()
197 str = strof_coding_type(coding); in hal_info_to_string()
206 MppCodingType coding = *((MppCodingType *)val); in hal_info_to_string() local
208 mpp_assert(coding == info->coding); in hal_info_to_string()
209 str = strof_coding_type(coding); in hal_info_to_string()
219 str = strof_profle(info->coding, profile); in hal_info_to_string()
[all …]
/rockchip-linux_mpp/mpp/codec/dec/av1/
H A Dav1d_parser2_syntax.c59 pp->coding.current_operating_point = seq->operating_point_idc[h->operating_point_idc]; in av1d_fill_picparams()
60 pp->coding.use_128x128_superblock = seq->use_128x128_superblock; in av1d_fill_picparams()
61 pp->coding.intra_edge_filter = seq->enable_intra_edge_filter; in av1d_fill_picparams()
62 pp->coding.interintra_compound = seq->enable_interintra_compound; in av1d_fill_picparams()
63 pp->coding.masked_compound = seq->enable_masked_compound; in av1d_fill_picparams()
64 pp->coding.warped_motion = frame_header->allow_warped_motion; in av1d_fill_picparams()
65 pp->coding.dual_filter = seq->enable_dual_filter; in av1d_fill_picparams()
66 pp->coding.jnt_comp = seq->enable_jnt_comp; in av1d_fill_picparams()
67 pp->coding.screen_content_tools = frame_header->allow_screen_content_tools; in av1d_fill_picparams()
68 pp->coding.integer_mv = frame_header->force_integer_mv; in av1d_fill_picparams()
[all …]
/rockchip-linux_mpp/mpp/codec/
H A Dmpp_enc_v2.c46 MppCodingType coding = cfg->coding; in mpp_enc_init_v2() local
91 enc_hal_cfg.coding = coding; in mpp_enc_init_v2()
99 ctrl_cfg.coding = coding; in mpp_enc_init_v2()
118 ret = hal_info_init(&p->hal_info, MPP_CTX_ENC, coding); in mpp_enc_init_v2()
124 p->coding = coding; in mpp_enc_init_v2()
155 p->cfg->base.coding = coding; in mpp_enc_init_v2()
260 strof_coding_type(enc->coding), getpid()); in mpp_enc_start_v2()
278 strof_coding_type(enc->coding), getpid()); in mpp_enc_start_async()
H A Dmpp_dec.c435 val = hal_info_to_string(hal_info, DEC_INFO_FORMAT, &dec->coding); in update_dec_hal_info()
496 MppCodingType coding; in mpp_dec_init() local
530 coding = cfg->coding; in mpp_dec_init()
563 coding, in mpp_dec_init()
604 mpp_slots_set_prop(packet_slots, SLOTS_CODING_TYPE, &coding); in mpp_dec_init()
605 mpp_slots_set_prop(frame_slots, SLOTS_CODING_TYPE, &coding); in mpp_dec_init()
613 coding, in mpp_dec_init()
626 ret = hal_info_init(&p->hal_info, MPP_CTX_DEC, coding); in mpp_dec_init()
632 p->coding = coding; in mpp_dec_init()
/rockchip-linux_mpp/mpp/hal/
H A Dmpp_enc_hal.c37 MppCodingType coding; member
61 if (cfg->coding == hw_enc_apis[i]->coding) { in mpp_enc_hal_init()
62 p->coding = cfg->coding; in mpp_enc_hal_init()
85 mpp_err_f("could not found coding type %d\n", cfg->coding); in mpp_enc_hal_init()
H A Dmpp_hal.c99 cfg->coding == hw_apis[i]->coding) { in mpp_hal_init()
114 mpp_err_f("could not found coding type %d\n", cfg->coding); in mpp_hal_init()
/rockchip-linux_mpp/mpp/
H A Dmpi.c24 MppCodingType coding; member
446 MPP_RET mpp_init(MppCtx ctx, MppCtxType type, MppCodingType coding) in mpp_init() argument
451 mpi_dbg_func("enter ctx %p type %d coding %d\n", ctx, type, coding); in mpp_init()
458 coding >= MPP_VIDEO_CodingMax) { in mpp_init()
459 mpp_err_f("invalid input type %d coding %d\n", type, coding); in mpp_init()
464 ret = mpp_ctx_init(p->ctx, type, coding); in mpp_init()
466 p->coding = coding; in mpp_init()
495 MPP_RET mpp_check_support_format(MppCtxType type, MppCodingType coding) in mpp_check_support_format() argument
503 coding == info->coding) { in mpp_check_support_format()
521 info->coding_name, info->coding); in mpp_show_support_format()
H A Dmpp.c63 static RK_S32 check_frm_task_cnt_cap(MppCodingType coding) in check_frm_task_cnt_cap() argument
68 if (coding == MPP_VIDEO_CodingAVC || coding == MPP_VIDEO_CodingHEVC) in check_frm_task_cnt_cap()
70 if (coding == MPP_VIDEO_CodingMJPEG && soc_type == ROCKCHIP_SOC_RK3588) in check_frm_task_cnt_cap()
150 MPP_RET mpp_ctx_init(Mpp *mpp, MppCtxType type, MppCodingType coding) in mpp_ctx_init() argument
159 if (!mpp_check_soc_cap(type, coding)) { in mpp_ctx_init()
161 strof_ctx_type(type), strof_coding_type(coding), in mpp_ctx_init()
166 if (mpp_check_support_format(type, coding)) { in mpp_ctx_init()
168 strof_ctx_type(type), strof_coding_type(coding)); in mpp_ctx_init()
172 mpp_ops_init(mpp->mDump, type, coding); in mpp_ctx_init()
175 mpp->mCoding = coding; in mpp_ctx_init()
[all …]
H A Dmpp_impl.c45 MppCodingType coding; member
63 MppCodingType coding; member
322 MPP_RET mpp_ops_init(MppDump info, MppCtxType type, MppCodingType coding) in mpp_ops_init() argument
332 p->coding = coding; in mpp_ops_init()
361 ops_log(p->fp_ops, "%d,%s,%d,%d\n", p->idx++, "init", type, coding); in mpp_ops_init()
/rockchip-linux_mpp/mpp/base/inc/
H A Dmpp_2str.h29 const char *strof_coding_type(MppCodingType coding);
31 const char *strof_profle(MppCodingType coding, RK_U32 profile);
/rockchip-linux_mpp/mpp/codec/inc/
H A Dparser_api.h34 MppCodingType coding; member
60 MppCodingType coding; member
H A Denc_impl_api.h32 MppCodingType coding; member
57 MppCodingType coding; member
/rockchip-linux_mpp/mpp/hal/rkdec/av1d/
H A Dhal_av1d_vdpu383.c1433 mpp_put_bits(&bp, dxva->coding.current_operating_point, 12); in prepare_uncompress_header()
1434 mpp_put_bits(&bp, dxva->coding.use_128x128_superblock, 1); in prepare_uncompress_header()
1435 mpp_put_bits(&bp, dxva->coding.filter_intra, 1); in prepare_uncompress_header()
1436 mpp_put_bits(&bp, dxva->coding.intra_edge_filter, 1); in prepare_uncompress_header()
1437 mpp_put_bits(&bp, dxva->coding.interintra_compound, 1); in prepare_uncompress_header()
1438 mpp_put_bits(&bp, dxva->coding.masked_compound, 1); in prepare_uncompress_header()
1439 mpp_put_bits(&bp, dxva->coding.dual_filter, 1); in prepare_uncompress_header()
1441 mpp_put_bits(&bp, dxva->coding.jnt_comp, 1); in prepare_uncompress_header()
1442 mpp_put_bits(&bp, dxva->coding.enable_ref_frame_mvs, 1); in prepare_uncompress_header()
1474 mpp_put_bits(&bp, dxva->coding.film_grain_en, 1); in prepare_uncompress_header()
[all …]
/rockchip-linux_mpp/mpp/hal/vpu/av1d/
H A Dhal_av1d_vdpu.c793 if (!dxva->coding.intrabc) { in vdpu_av1d_set_reference_frames()
814 if (dxva->coding.intrabc) { in vdpu_av1d_set_reference_frames()
868 if (dxva->coding.intrabc) { in vdpu_av1d_set_reference_frames()
1021 if (dxva->coding.use_ref_frame_mvs && ref_ind > 0 && in vdpu_av1d_set_reference_frames()
1028 if (dxva->coding.use_ref_frame_mvs && ref_ind > 1 && in vdpu_av1d_set_reference_frames()
1035 if (dxva->coding.use_ref_frame_mvs && ref_ind > 2 && in vdpu_av1d_set_reference_frames()
1123 if (dxva->coding.superres) { in vdpu_av1d_superres_params()
1243 regs->swreg5.sw_error_resilient = dxva->coding.error_resilient_mode; in vdpu_av1d_set_segmentation()
1499 …if (!leftmost && dxva->coding.use_128x128_superblock == 0 && dxva->coding.superres && width == 1) { in check_tile_width()
1504 const RK_S32 sb_size_log2 = dxva->coding.use_128x128_superblock ? 7 : 6; in check_tile_width()
[all …]
/rockchip-linux_mpp/mpp/hal/inc/
H A Dmpp_hal.h41 MppCodingType coding; member
58 MppCodingType coding; member
H A Dmpp_enc_hal.h26 MppCodingType coding; member
40 MppCodingType coding; member
/rockchip-linux_mpp/inc/
H A Drk_mpi.h242 MPP_RET mpp_init(MppCtx ctx, MppCtxType type, MppCodingType coding);
259 MPP_RET mpp_check_support_format(MppCtxType type, MppCodingType coding);
/rockchip-linux_mpp/test/
H A Dvpu_api_test.c42 OMX_RK_VIDEO_CODINGTYPE coding; member
189 cmdCxt->coding = atoi(argv[optindex]); in parse_options()
261 || (cmd->coding <= OMX_RK_VIDEO_CodingAutoDetect)) { in vpu_encode_demo()
267 cmd->width, cmd->height, cmd->coding, in vpu_encode_demo()
330 ctx->videoCoding = cmd->coding; in vpu_encode_demo()
517 || (cmd->coding <= OMX_RK_VIDEO_CodingAutoDetect)) { in vpu_decode_demo()
523 cmd->width, cmd->height, cmd->coding, in vpu_decode_demo()
591 ctx->videoCoding = cmd->coding; in vpu_decode_demo()
/rockchip-linux_mpp/mpp/legacy/
H A Dvpu.c128 MppCodingType coding = MPP_VIDEO_CodingAutoDetect; in VPUClientInit() local
132 coding = MPP_VIDEO_CodingHEVC; in VPUClientInit()
137 coding = MPP_VIDEO_CodingAVSPLUS; in VPUClientInit()
159 path = mpp_get_vcodec_dev_name(ctx_type, coding); in VPUClientInit()
/rockchip-linux_mpp/mpp/codec/dec/vp8/
H A Dvp8d_api.c28 .coding = MPP_VIDEO_CodingVP8,
/rockchip-linux_mpp/mpp/codec/dec/m2v/
H A Dm2vd_api.c27 .coding = MPP_VIDEO_CodingMPEG2,

12345