/device/soc/winnermicro/wm800/board/src/bt/blehost/nimble/host/src/ |
D | ble_att_cmd.c | 94 void ble_att_error_rsp_parse(const void *payload, int len, struct ble_att_error_rsp *dst) in ble_att_error_rsp_parse() argument 99 dst->baep_req_op = src->baep_req_op; in ble_att_error_rsp_parse() 100 dst->baep_handle = le16toh(src->baep_handle); in ble_att_error_rsp_parse() 101 dst->baep_error_code = src->baep_error_code; in ble_att_error_rsp_parse() 106 struct ble_att_error_rsp *dst; in ble_att_error_rsp_write() local 107 dst = ble_att_init_write(BLE_ATT_OP_ERROR_RSP, payload, in ble_att_error_rsp_write() 109 dst->baep_req_op = src->baep_req_op; in ble_att_error_rsp_write() 110 dst->baep_handle = htole16(src->baep_handle); in ble_att_error_rsp_write() 111 dst->baep_error_code = src->baep_error_code; in ble_att_error_rsp_write() 114 void ble_att_mtu_req_parse(const void *payload, int len, struct ble_att_mtu_cmd *dst) in ble_att_mtu_req_parse() argument [all …]
|
D | ble_uuid.c | 96 void ble_uuid_copy(ble_uuid_any_t *dst, const ble_uuid_t *src) in ble_uuid_copy() argument 102 dst->u16 = *(const ble_uuid16_t *)src; in ble_uuid_copy() 106 dst->u32 = *(const ble_uuid32_t *)src; in ble_uuid_copy() 110 dst->u128 = *(const ble_uuid128_t *)src; in ble_uuid_copy() 119 char *ble_uuid_to_str(const ble_uuid_t *uuid, char *dst) in ble_uuid_to_str() argument 125 sprintf_s(dst, sizeof(*dst), "0x%04x", BLE_UUID16(uuid)->value); in ble_uuid_to_str() 129 sprintf_s(dst, sizeof(*dst), "0x%08x", BLE_UUID32(uuid)->value); in ble_uuid_to_str() 134 sprintf_s(dst, sizeof(*dst), "%02x%02x%02x%02x-%02x%02x-%02x%02x-%02x%02x-" in ble_uuid_to_str() 147 dst[0] = '\0'; in ble_uuid_to_str() 151 return dst; in ble_uuid_to_str() [all …]
|
D | ble_hs_adv.c | 37 uint8_t *dst, uint8_t *dst_len, struct os_mbuf *om) in ble_hs_adv_set_hdr() argument 54 dst[*dst_len] = data_len_tmp + 1; in ble_hs_adv_set_hdr() 55 dst[*dst_len + 1] = type; in ble_hs_adv_set_hdr() 61 uint8_t *dst, uint8_t *dst_len, uint8_t max_len, in ble_hs_adv_set_flat_mbuf() argument 66 rc = ble_hs_adv_set_hdr(type, data_len, max_len, dst, dst_len, om); in ble_hs_adv_set_flat_mbuf() 75 memcpy_s(dst + *dst_len, sizeof(dst + *dst_len), data, data_len); in ble_hs_adv_set_flat_mbuf() 81 uint8_t *dst, uint8_t *dst_len, uint8_t max_len) in ble_hs_adv_set_flat() argument 86 return ble_hs_adv_set_flat_mbuf(type, data_len, data, dst, dst_len, max_len, in ble_hs_adv_set_flat() 91 const ble_uuid16_t *elems, uint8_t *dst, in ble_hs_adv_set_array_uuid16() argument 97 rc = ble_hs_adv_set_hdr(type, num_elems * 2, max_len, dst, // 2:byte alignment in ble_hs_adv_set_array_uuid16() [all …]
|
/device/board/isoftstone/zhiyuan/kernel/driver/drivers/g2d/g2d_rcq/ |
D | g2d_rotate.c | 106 __s32 g2d_rotate_set_para(g2d_image_enh *src, g2d_image_enh *dst, __u32 flag) in g2d_rotate_set_para() argument 117 if (!dst || g2d_image_check(dst)) in g2d_rotate_set_para() 122 if (!src->use_phy_addr || !dst->use_phy_addr) { in g2d_rotate_set_para() 144 ret = g2d_dma_map(dst->fd, dst_item); in g2d_rotate_set_para() 149 g2d_set_info(dst, dst_item); in g2d_rotate_set_para() 224 dst->clip_rect.w = src->clip_rect.h; in g2d_rotate_set_para() 225 dst->clip_rect.h = src->clip_rect.w; in g2d_rotate_set_para() 229 dst->clip_rect.w = src->clip_rect.w; in g2d_rotate_set_para() 230 dst->clip_rect.h = src->clip_rect.h; in g2d_rotate_set_para() 232 write_wvalue(ROT_OSIZE, ((((dst->clip_rect.h - 1) & 0x1fff) << 16)) | in g2d_rotate_set_para() [all …]
|
D | g2d_mixer.c | 26 g2d_image_enh *mask, g2d_image_enh *dst, in g2d_bsp_maskblt() argument 32 if (!dst) { in g2d_bsp_maskblt() 37 if (dst->format > G2D_FORMAT_BGRA1010102) { in g2d_bsp_maskblt() 38 G2D_ERR_MSG("Un support out format:%d\n", dst->format); in g2d_bsp_maskblt() 41 g2d_vlayer_set(p_frame->ovl_v, 0, dst); in g2d_bsp_maskblt() 44 src->clip_rect.w = dst->clip_rect.w; in g2d_bsp_maskblt() 45 src->clip_rect.h = dst->clip_rect.h; in g2d_bsp_maskblt() 49 ptn->clip_rect.w = dst->clip_rect.w; in g2d_bsp_maskblt() 50 ptn->clip_rect.h = dst->clip_rect.h; in g2d_bsp_maskblt() 55 mask->clip_rect.w = dst->clip_rect.w; in g2d_bsp_maskblt() [all …]
|
/device/soc/rockchip/rk3568/hardware/omx_il/osal/ |
D | Rockchip_OSAL_RGA_Process.c | 124 Rga_Request.dst.yrgb_addr = 0; in rga_copy() 127 Rga_Request.dst.yrgb_addr = vpumem->phy_addr; in rga_copy() 130 Rga_Request.dst.uv_addr = vpumem->vir_addr; in rga_copy() 135 Rga_Request.dst.uv_addr = vpumem->phy_addr; in rga_copy() 137 Rga_Request.dst.yrgb_addr = vpumem->phy_addr; in rga_copy() 138 Rga_Request.dst.uv_addr = (unsigned long)vpumem->vir_addr; in rga_copy() 141 Rga_Request.dst.v_addr = 0; in rga_copy() 142 Rga_Request.dst.vir_w = Width; in rga_copy() 143 Rga_Request.dst.vir_h = Height; in rga_copy() 144 Rga_Request.dst.format = Rga_Request.src.format; in rga_copy() [all …]
|
/device/board/isoftstone/zhiyuan/kernel/driver/drivers/g2d/g2d_legacy/ |
D | g2d_bsp_v2.c | 1400 g2d_image_enh *dst = &dst_tmp; in mixer_fillrectangle() local 1406 dst->bbuff = 1; in mixer_fillrectangle() 1407 dst->color = para->color; in mixer_fillrectangle() 1408 dst->format = in mixer_fillrectangle() 1411 dst->laddr[0] = para->dst_image.addr[0]; in mixer_fillrectangle() 1412 dst->laddr[1] = para->dst_image.addr[1]; in mixer_fillrectangle() 1413 dst->laddr[2] = para->dst_image.addr[2]; in mixer_fillrectangle() 1414 dst->width = para->dst_image.w; in mixer_fillrectangle() 1415 dst->height = para->dst_image.h; in mixer_fillrectangle() 1416 dst->clip_rect.x = para->dst_rect.x; in mixer_fillrectangle() [all …]
|
/device/soc/rockchip/rk3588/hardware/rga/include/ |
D | im2d.h | 191 #define imcheck(src, dst, src_rect, dst_rect, ...) \ argument 201 … rga_check_perpare((rga_buffer_t *)(&src), (rga_buffer_t *)(&dst), (rga_buffer_t *)(&__pat), \ 203 __ret = imcheck_t(src, dst, __pat, src_rect, dst_rect, __pat_rect, 0); \ 205 … rga_check_perpare((rga_buffer_t *)(&src), (rga_buffer_t *)(&dst), (rga_buffer_t *)(&__pat), \ 207 __ret = imcheck_t(src, dst, __pat, src_rect, dst_rect, __pat_rect, __args[0]); \ 214 #define imcheck_composite(src, dst, pat, src_rect, dst_rect, pat_rect, ...) \ argument 220 … rga_check_perpare((rga_buffer_t *)(&src), (rga_buffer_t *)(&dst), (rga_buffer_t *)(&pat), \ 222 __ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); \ 224 … rga_check_perpare((rga_buffer_t *)(&src), (rga_buffer_t *)(&dst), (rga_buffer_t *)(&pat), \ 226 __ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, __args[0]); \ [all …]
|
/device/soc/allwinner/t507/hardware/rga/include/ |
D | im2d.h | 375 #define imcheck(src, dst, src_rect, dst_rect, ...) \ argument 391 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); \ 393 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, args[0]); \ 400 #define imcheck_composite(src, dst, pat, src_rect, dst_rect, pat_rect, ...) \ argument 406 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); \ 408 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, args[0]); \ 415 IM_API IM_STATUS imcheck_t(const rga_buffer_t src, const rga_buffer_t dst, const rga_buffer_t pat, 432 #define imresize(src, dst, ...) \ argument 438 ret = imresize_t(src, dst, 0, 0, INTER_LINEAR, 1); \ 440 ret = imresize_t(src, dst, args[0], args[1], INTER_LINEAR, 1); \ [all …]
|
/device/soc/rockchip/common/hardware/rga/include/ |
D | im2d.h | 375 #define imcheck(src, dst, src_rect, dst_rect, ...) … argument 391 …ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); … 393 …ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, args[0]); … 400 #define imcheck_composite(src, dst, pat, src_rect, dst_rect, pat_rect, ...) … argument 406 …ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); … 408 …ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, args[0]); … 415 IM_API IM_STATUS imcheck_t(const rga_buffer_t src, const rga_buffer_t dst, const rga_buffer_t pat, 432 #define imresize(src, dst, ...) … argument 438 …ret = imresize_t(src, dst, 0, 0, INTER_LINEAR, 1); … 440 …ret = imresize_t(src, dst, args[0], args[1], INTER_LINEAR, 1); … [all …]
|
/device/soc/rockchip/rk3568/hardware/rga/include/ |
D | im2d.h | 385 #define imcheck(src, dst, src_rect, dst_rect, ...) \ argument 401 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); \ 403 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, args[0]); \ 410 #define imcheck_composite(src, dst, pat, src_rect, dst_rect, pat_rect, ...) \ argument 416 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); \ 418 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, args[0]); \ 425 IM_API IM_STATUS imcheck_t(const rga_buffer_t src, const rga_buffer_t dst, const rga_buffer_t pat, 442 #define imresize(src, dst, ...) \ argument 448 ret = imresize_t(src, dst, 0, 0, INTER_LINEAR, 1); \ 450 ret = imresize_t(src, dst, args[0], args[1], INTER_LINEAR, 1); \ [all …]
|
/device/soc/rockchip/rk3399/hardware/rga/include/ |
D | im2d.h | 385 #define imcheck(src, dst, src_rect, dst_rect, ...) \ argument 401 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); \ 403 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, args[0]); \ 410 #define imcheck_composite(src, dst, pat, src_rect, dst_rect, pat_rect, ...) \ argument 416 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, 0); \ 418 ret = imcheck_t(src, dst, pat, src_rect, dst_rect, pat_rect, args[0]); \ 425 IM_API IM_STATUS imcheck_t(const rga_buffer_t src, const rga_buffer_t dst, const rga_buffer_t pat, 442 #define imresize(src, dst, ...) \ argument 448 ret = imresize_t(src, dst, 0, 0, INTER_LINEAR, 1); \ 450 ret = imresize_t(src, dst, args[0], args[1], INTER_LINEAR, 1); \ [all …]
|
/device/soc/winnermicro/wm800/board/include/platform/ |
D | wm_mem.h | 81 #define MEMCPY(dst, src, len) do { \ argument 82 if (tls_is_safe_addr(dst, len)) { \ 83 memcpy_s(dst, sizeof(dst), src, len);}}while (0) 85 #define SMEMCPY(dst, src, len) do { \ argument 86 if (tls_is_safe_addr(dst, len)) { \ 87 memcpy_s(dst, sizeof(dst), src, len);}}while (0) 174 #define MEMCPY(dst, src, len) memcpy(dst, src, len) argument 187 #define SMEMCPY(dst, src, len) memcpy_s(dst, sizeof(dst), src, len) argument 203 #define MEMCPY(dst, src, len) memcpy_s(dst, sizeof(dst), src, len) argument 204 #define SMEMCPY(dst, src, len) memcpy_s(dst, sizeof(dst), src, len) argument
|
/device/soc/rockchip/common/kernel/drivers/gpu/arm/bifrost/ |
D | mali_kbase_hwcnt_types.c | 305 struct kbase_hwcnt_dump_buffer *dst, in kbase_hwcnt_dump_buffer_zero() argument 311 if (WARN_ON(!dst) || in kbase_hwcnt_dump_buffer_zero() 313 WARN_ON(dst->metadata != dst_enable_map->metadata)) in kbase_hwcnt_dump_buffer_zero() 316 metadata = dst->metadata; in kbase_hwcnt_dump_buffer_zero() 327 dst, grp, blk, blk_inst); in kbase_hwcnt_dump_buffer_zero() 334 memset(dst->clk_cnt_buf, 0, in kbase_hwcnt_dump_buffer_zero() 335 sizeof(*dst->clk_cnt_buf) * metadata->clk_cnt); in kbase_hwcnt_dump_buffer_zero() 339 struct kbase_hwcnt_dump_buffer *dst) in kbase_hwcnt_dump_buffer_zero_strict() argument 341 if (WARN_ON(!dst)) in kbase_hwcnt_dump_buffer_zero_strict() 344 memset(dst->dump_buf, 0, dst->metadata->dump_buf_bytes); in kbase_hwcnt_dump_buffer_zero_strict() [all …]
|
D | mali_kbase_hwcnt_gpu.c | 29 static void kbasep_get_fe_block_type(u64 *dst, enum kbase_hwcnt_set counter_set, in kbasep_get_fe_block_type() argument 34 *dst = KBASE_HWCNT_GPU_V5_BLOCK_TYPE_PERF_FE; in kbasep_get_fe_block_type() 38 *dst = KBASE_HWCNT_GPU_V5_BLOCK_TYPE_PERF_FE2; in kbasep_get_fe_block_type() 40 *dst = KBASE_HWCNT_GPU_V5_BLOCK_TYPE_PERF_UNDEFINED; in kbasep_get_fe_block_type() 45 *dst = KBASE_HWCNT_GPU_V5_BLOCK_TYPE_PERF_FE3; in kbasep_get_fe_block_type() 47 *dst = KBASE_HWCNT_GPU_V5_BLOCK_TYPE_PERF_UNDEFINED; in kbasep_get_fe_block_type() 55 static void kbasep_get_tiler_block_type(u64 *dst, in kbasep_get_tiler_block_type() argument 60 *dst = KBASE_HWCNT_GPU_V5_BLOCK_TYPE_PERF_TILER; in kbasep_get_tiler_block_type() 64 *dst = KBASE_HWCNT_GPU_V5_BLOCK_TYPE_PERF_UNDEFINED; in kbasep_get_tiler_block_type() 71 static void kbasep_get_sc_block_type(u64 *dst, enum kbase_hwcnt_set counter_set, in kbasep_get_sc_block_type() argument [all …]
|
/device/soc/rockchip/common/vendor/drivers/gpu/arm/bifrost/ |
D | mali_kbase_hwcnt_types.c | 307 void kbase_hwcnt_dump_buffer_zero(struct kbase_hwcnt_dump_buffer *dst, in kbase_hwcnt_dump_buffer_zero() argument 313 …if (WARN_ON(!dst) || WARN_ON(!dst_enable_map) || WARN_ON(dst->metadata != dst_enable_map->metadata… in kbase_hwcnt_dump_buffer_zero() 317 metadata = dst->metadata; in kbase_hwcnt_dump_buffer_zero() 328 dst_blk = kbase_hwcnt_dump_buffer_block_instance(dst, grp, blk, blk_inst); in kbase_hwcnt_dump_buffer_zero() 334 memset(dst->clk_cnt_buf, 0, sizeof(*dst->clk_cnt_buf) * metadata->clk_cnt); in kbase_hwcnt_dump_buffer_zero() 338 void kbase_hwcnt_dump_buffer_zero_strict(struct kbase_hwcnt_dump_buffer *dst) in kbase_hwcnt_dump_buffer_zero_strict() argument 340 if (WARN_ON(!dst)) { in kbase_hwcnt_dump_buffer_zero_strict() 344 memset(dst->dump_buf, 0, dst->metadata->dump_buf_bytes); in kbase_hwcnt_dump_buffer_zero_strict() 346 memset(dst->clk_cnt_buf, 0, sizeof(*dst->clk_cnt_buf) * dst->metadata->clk_cnt); in kbase_hwcnt_dump_buffer_zero_strict() 350 void kbase_hwcnt_dump_buffer_zero_non_enabled(struct kbase_hwcnt_dump_buffer *dst, in kbase_hwcnt_dump_buffer_zero_non_enabled() argument [all …]
|
/device/soc/esp/esp32/components/bt/common/btc/profile/esp/blufi/ |
D | blufi_prf.c | 419 esp_blufi_cb_param_t *dst = (esp_blufi_cb_param_t *) p_dest; in btc_blufi_cb_deep_copy() local 424 dst->sta_ssid.ssid = osi_malloc(src->sta_ssid.ssid_len); in btc_blufi_cb_deep_copy() 425 if (dst->sta_ssid.ssid == NULL) { in btc_blufi_cb_deep_copy() 428 memcpy(dst->sta_ssid.ssid, src->sta_ssid.ssid, src->sta_ssid.ssid_len); in btc_blufi_cb_deep_copy() 431 dst->sta_passwd.passwd = osi_malloc(src->sta_passwd.passwd_len); in btc_blufi_cb_deep_copy() 432 if (dst->sta_passwd.passwd == NULL) { in btc_blufi_cb_deep_copy() 435 memcpy(dst->sta_passwd.passwd, src->sta_passwd.passwd, src->sta_passwd.passwd_len); in btc_blufi_cb_deep_copy() 438 dst->softap_ssid.ssid = osi_malloc(src->softap_ssid.ssid_len); in btc_blufi_cb_deep_copy() 439 if (dst->softap_ssid.ssid == NULL) { in btc_blufi_cb_deep_copy() 442 memcpy(dst->softap_ssid.ssid, src->softap_ssid.ssid, src->softap_ssid.ssid_len); in btc_blufi_cb_deep_copy() [all …]
|
/device/board/isoftstone/yangfan/common/seetafaceengine/opencv2/3rdparty/carotene/hal/ |
D | tegra_hal.hpp | 119 #define TEGRA_BINARYOP(type, op, src1, sz1, src2, sz2, dst, sz, w, h) \ argument 123 TegraGenOp_##op##_Invoker<const type, type>(src1, sz1, src2, sz2, dst, sz, w, h), \ 154 #define TEGRA_UNARYOP(type, op, src1, sz1, dst, sz, w, h) \ argument 158 TegraGenOp_##op##_Invoker<const type, type>(src1, sz1, dst, sz, w, h), \ 165 …ne cv_hal_add8u(src1, sz1, src2, sz2, dst, sz, w, h) TEGRA_BINARYOP(CAROTENE_NS::u8, add, src1, sz… argument 167 …ne cv_hal_add8s(src1, sz1, src2, sz2, dst, sz, w, h) TEGRA_BINARYOP(CAROTENE_NS::s8, add, src1, sz… argument 169 … cv_hal_add16u(src1, sz1, src2, sz2, dst, sz, w, h) TEGRA_BINARYOP(CAROTENE_NS::u16, add, src1, sz… argument 171 … cv_hal_add16s(src1, sz1, src2, sz2, dst, sz, w, h) TEGRA_BINARYOP(CAROTENE_NS::s16, add, src1, sz… argument 173 … cv_hal_add32s(src1, sz1, src2, sz2, dst, sz, w, h) TEGRA_BINARYOP(CAROTENE_NS::s32, add, src1, sz… argument 175 … cv_hal_add32f(src1, sz1, src2, sz2, dst, sz, w, h) TEGRA_BINARYOP(CAROTENE_NS::f32, addf, src1, s… argument [all …]
|
/device/soc/rockchip/common/vendor/drivers/video/rockchip/rga2/ |
D | rga2_reg_info.c | 59 dw = msg->dst.act_h; in RGA2_reg_get_param() 60 dh = msg->dst.act_w; in RGA2_reg_get_param() 62 dw = msg->dst.act_w; in RGA2_reg_get_param() 63 dh = msg->dst.act_h; in RGA2_reg_get_param() 181 …if ((msg->src.act_w == msg->dst.act_w) && (msg->src.act_h == msg->dst.act_h) && (msg->rotate_mode … in RGA2_set_reg_src_info() 193 dw = msg->dst.act_h; in RGA2_set_reg_src_info() 194 dh = msg->dst.act_w; in RGA2_set_reg_src_info() 196 dw = msg->dst.act_w; in RGA2_set_reg_src_info() 197 dh = msg->dst.act_h; in RGA2_set_reg_src_info() 685 switch (msg->dst.format) { in RGA2_set_reg_dst_info() [all …]
|
D | rga2_mmu_info.c | 344 struct rga_img_info_t *src0, *src1, *dst, *els; in rga2_get_dma_info() local 358 dst = &req->dst; in rga2_get_dma_info() 410 if (unlikely(!mmu_flag && dst->yrgb_addr)) { in rga2_get_dma_info() 414 } else if (mmu_flag && dst->yrgb_addr) { in rga2_get_dma_info() 415 ret = rga2_map_dma_buffer(dst->yrgb_addr, buffer_dst, DMA_BIDIRECTIONAL); in rga2_get_dma_info() 423 ret = rga2_dma_memory_check(buffer_dst, dst); in rga2_get_dma_info() 430 rga2_convert_addr(dst); in rga2_get_dma_info() 487 dst_vir_w = req->dst.vir_w; in rga2_get_dma_info() 528 if ((int)req->dst.yrgb_addr > 0) { in rga2_get_dma_info() 529 hdl = ion_import_dma_buf(rga2_drvdata->ion_client, req->dst.yrgb_addr); in rga2_get_dma_info() [all …]
|
/device/board/isoftstone/yangfan/kernel/src/driv/video/rockchip/rga2/ |
D | rga2_reg_info.c | 61 dw = msg->dst.act_h; in RGA2_reg_get_param() 62 dh = msg->dst.act_w; in RGA2_reg_get_param() 66 dw = msg->dst.act_w; in RGA2_reg_get_param() 67 dh = msg->dst.act_h; in RGA2_reg_get_param() 196 if ((msg->src.act_w == msg->dst.act_w) && in RGA2_set_reg_src_info() 197 (msg->src.act_h == msg->dst.act_h) && in RGA2_set_reg_src_info() 210 dw = msg->dst.act_h; in RGA2_set_reg_src_info() 211 dh = msg->dst.act_w; in RGA2_set_reg_src_info() 215 dw = msg->dst.act_w; in RGA2_set_reg_src_info() 216 dh = msg->dst.act_h; in RGA2_set_reg_src_info() [all …]
|
/device/soc/rockchip/rk3588/kernel/drivers/video/rockchip/rga3/ |
D | rga2_reg_info.c | 112 dw = msg->dst.act_h; in RGA2_reg_get_param() 113 dh = msg->dst.act_w; in RGA2_reg_get_param() 115 dw = msg->dst.act_w; in RGA2_reg_get_param() 116 dh = msg->dst.act_h; in RGA2_reg_get_param() 238 if ((msg->src.act_w == msg->dst.act_w) && in RGA2_set_reg_src_info() 239 (msg->src.act_h == msg->dst.act_h) && in RGA2_set_reg_src_info() 251 dw = msg->dst.act_h; in RGA2_set_reg_src_info() 252 dh = msg->dst.act_w; in RGA2_set_reg_src_info() 254 dw = msg->dst.act_w; in RGA2_set_reg_src_info() 255 dh = msg->dst.act_h; in RGA2_set_reg_src_info() [all …]
|
/device/board/isoftstone/yangfan/common/seetafaceengine/opencv2/3rdparty/carotene/src/ |
D | convert_depth.cpp | 61 s16 * dst = internal::getRowPtr(dstBase, dstStride, i); in lshiftConst() local 71 vst1q_s16(dst + j, vshlq_n_s16(v_dst0, shift)); in lshiftConst() 72 vst1q_s16(dst + j + 8, vshlq_n_s16(v_dst1, shift)); in lshiftConst() 77 vst1q_s16(dst + j, vshlq_n_s16(v_dst, shift)); in lshiftConst() 82 dst[j] = ((s16)src[j] << shift); in lshiftConst() 98 s16 * dst = internal::getRowPtr(dstBase, dstStride, i); in lshiftConst() local 108 vst1q_s16(dst + j, v_dst0); in lshiftConst() 109 vst1q_s16(dst + j + 8, v_dst1); in lshiftConst() 114 vst1q_s16(dst + j, v_dst); in lshiftConst() 119 dst[j] = (s16)src[j]; in lshiftConst() [all …]
|
D | accumulate.cpp | 60 s16* dst = internal::getRowPtr(dstBase, dstStride, i); in accumulate() local 66 internal::prefetch(dst + j); in accumulate() 68 int16x8_t v_dst0 = vld1q_s16(dst + j); in accumulate() 69 int16x8_t v_dst1 = vld1q_s16(dst + j + 8); in accumulate() 74 vst1q_s16(dst + j, v_dst0); in accumulate() 75 vst1q_s16(dst + j + 8, v_dst1); in accumulate() 81 int16x8_t v_dst = vld1q_s16(dst + j); in accumulate() 83 vst1q_s16(dst + j, v_dst); in accumulate() 87 dst[j] = internal::saturate_cast<s16>(src[j] + dst[j]); in accumulate() 113 s16* dst = internal::getRowPtr(dstBase, dstStride, i); in accumulateSquareConst() local [all …]
|
/device/soc/telink/b91/b91_ble_sdk/common/ |
D | utility.c | 34 void swapX(const u8 *src, u8 *dst, int len) in swapX() argument 38 dst[len - 1 - i] = src[i]; in swapX() 42 void swap24(u8 dst[3], const u8 src[3]) in swap24() 44 swapX(src, dst, 3); in swap24() 47 void swap32(u8 dst[4], const u8 src[4]) in swap32() 49 swapX(src, dst, 4); in swap32() 52 void swap48(u8 dst[7], const u8 src[7]) in swap48() 54 swapX(src, dst, 6); in swap48() 57 void swap56(u8 dst[7], const u8 src[7]) in swap56() 59 swapX(src, dst, 7); in swap56() [all …]
|