| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/hal/ |
| H A D | hal.hpp | 72 CV_EXPORTS void gemm32f(const float* src1, size_t src1_step, const float* src2, size_t src2_step, 75 CV_EXPORTS void gemm64f(const double* src1, size_t src1_step, const double* src2, size_t src2_step, 78 CV_EXPORTS void gemm32fc(const float* src1, size_t src1_step, const float* src2, size_t src2_step, 81 CV_EXPORTS void gemm64fc(const double* src1, size_t src1_step, const double* src2, size_t src2_step, 113 CV_EXPORTS void add8u( const uchar* src1, size_t step1, const uchar* src2, size_t step2, uchar* dst… 114 CV_EXPORTS void add8s( const schar* src1, size_t step1, const schar* src2, size_t step2, schar* dst… 115 CV_EXPORTS void add16u( const ushort* src1, size_t step1, const ushort* src2, size_t step2, ushort*… 116 CV_EXPORTS void add16s( const short* src1, size_t step1, const short* src2, size_t step2, short* ds… 117 CV_EXPORTS void add32s( const int* src1, size_t step1, const int* src2, size_t step2, int* dst, siz… 118 CV_EXPORTS void add32f( const float* src1, size_t step1, const float* src2, size_t step2, float* ds… [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/hal/ |
| H A D | hal.hpp | 72 CV_EXPORTS void gemm32f(const float* src1, size_t src1_step, const float* src2, size_t src2_step, 75 CV_EXPORTS void gemm64f(const double* src1, size_t src1_step, const double* src2, size_t src2_step, 78 CV_EXPORTS void gemm32fc(const float* src1, size_t src1_step, const float* src2, size_t src2_step, 81 CV_EXPORTS void gemm64fc(const double* src1, size_t src1_step, const double* src2, size_t src2_step, 113 CV_EXPORTS void add8u( const uchar* src1, size_t step1, const uchar* src2, size_t step2, uchar* dst… 114 CV_EXPORTS void add8s( const schar* src1, size_t step1, const schar* src2, size_t step2, schar* dst… 115 CV_EXPORTS void add16u( const ushort* src1, size_t step1, const ushort* src2, size_t step2, ushort*… 116 CV_EXPORTS void add16s( const short* src1, size_t step1, const short* src2, size_t step2, short* ds… 117 CV_EXPORTS void add32s( const int* src1, size_t step1, const int* src2, size_t step2, int* dst, siz… 118 CV_EXPORTS void add32f( const float* src1, size_t step1, const float* src2, size_t step2, float* ds… [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/hal/ |
| H A D | hal.hpp | 72 CV_EXPORTS void gemm32f(const float* src1, size_t src1_step, const float* src2, size_t src2_step, 75 CV_EXPORTS void gemm64f(const double* src1, size_t src1_step, const double* src2, size_t src2_step, 78 CV_EXPORTS void gemm32fc(const float* src1, size_t src1_step, const float* src2, size_t src2_step, 81 CV_EXPORTS void gemm64fc(const double* src1, size_t src1_step, const double* src2, size_t src2_step, 113 CV_EXPORTS void add8u( const uchar* src1, size_t step1, const uchar* src2, size_t step2, uchar* dst… 114 CV_EXPORTS void add8s( const schar* src1, size_t step1, const schar* src2, size_t step2, schar* dst… 115 CV_EXPORTS void add16u( const ushort* src1, size_t step1, const ushort* src2, size_t step2, ushort*… 116 CV_EXPORTS void add16s( const short* src1, size_t step1, const short* src2, size_t step2, short* ds… 117 CV_EXPORTS void add32s( const int* src1, size_t step1, const int* src2, size_t step2, int* dst, siz… 118 CV_EXPORTS void add32f( const float* src1, size_t step1, const float* src2, size_t step2, float* ds… [all …]
|
| /OK3568_Linux_fs/kernel/drivers/crypto/caam/ |
| H A D | desc_constr.h | 415 #define append_math_add(desc, dest, src0, src1, len) \ argument 416 APPEND_MATH(ADD, desc, dest, src0, src1, len) 417 #define append_math_sub(desc, dest, src0, src1, len) \ argument 418 APPEND_MATH(SUB, desc, dest, src0, src1, len) 419 #define append_math_add_c(desc, dest, src0, src1, len) \ argument 420 APPEND_MATH(ADDC, desc, dest, src0, src1, len) 421 #define append_math_sub_b(desc, dest, src0, src1, len) \ argument 422 APPEND_MATH(SUBB, desc, dest, src0, src1, len) 423 #define append_math_and(desc, dest, src0, src1, len) \ argument 424 APPEND_MATH(AND, desc, dest, src0, src1, len) [all …]
|
| /OK3568_Linux_fs/kernel/arch/powerpc/include/asm/ |
| H A D | kvm_fpu.h | 14 extern void fps_fres(u64 *fpscr, u32 *dst, u32 *src1); 15 extern void fps_frsqrte(u64 *fpscr, u32 *dst, u32 *src1); 16 extern void fps_fsqrts(u64 *fpscr, u32 *dst, u32 *src1); 18 extern void fps_fadds(u64 *fpscr, u32 *dst, u32 *src1, u32 *src2); 19 extern void fps_fdivs(u64 *fpscr, u32 *dst, u32 *src1, u32 *src2); 20 extern void fps_fmuls(u64 *fpscr, u32 *dst, u32 *src1, u32 *src2); 21 extern void fps_fsubs(u64 *fpscr, u32 *dst, u32 *src1, u32 *src2); 23 extern void fps_fmadds(u64 *fpscr, u32 *dst, u32 *src1, u32 *src2, 25 extern void fps_fmsubs(u64 *fpscr, u32 *dst, u32 *src1, u32 *src2, 27 extern void fps_fnmadds(u64 *fpscr, u32 *dst, u32 *src1, u32 *src2, [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/cuda/detail/ |
| H A D | transform_detail.hpp | 84 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 87 dst.x = op(src1.x, src2.x); in unroll() 102 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 105 dst.x = op(src1.x, src2.x); in unroll() 107 dst.y = op(src1.y, src2.y); in unroll() 124 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 127 dst.x = op(src1.x, src2.x); in unroll() 129 dst.y = op(src1.y, src2.y); in unroll() 131 dst.z = op(src1.z, src2.z); in unroll() 150 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/cuda/detail/ |
| H A D | transform_detail.hpp | 84 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 87 dst.x = op(src1.x, src2.x); in unroll() 102 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 105 dst.x = op(src1.x, src2.x); in unroll() 107 dst.y = op(src1.y, src2.y); in unroll() 124 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 127 dst.x = op(src1.x, src2.x); in unroll() 129 dst.y = op(src1.y, src2.y); in unroll() 131 dst.z = op(src1.z, src2.z); in unroll() 150 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/cuda/detail/ |
| H A D | transform_detail.hpp | 84 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 87 dst.x = op(src1.x, src2.x); in unroll() 102 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 105 dst.x = op(src1.x, src2.x); in unroll() 107 dst.y = op(src1.y, src2.y); in unroll() 124 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() 127 dst.x = op(src1.x, src2.x); in unroll() 129 dst.y = op(src1.y, src2.y); in unroll() 131 dst.z = op(src1.z, src2.z); in unroll() 150 …static __device__ __forceinline__ void unroll(const T1& src1, const T2& src2, D& dst, const Mask& … in unroll() [all …]
|
| /OK3568_Linux_fs/kernel/include/linux/ |
| H A D | bitmap.h | 141 extern bool __pure __bitmap_or_equal(const unsigned long *src1, 291 static inline int bitmap_and(unsigned long *dst, const unsigned long *src1, in bitmap_and() argument 295 return (*dst = *src1 & *src2 & BITMAP_LAST_WORD_MASK(nbits)) != 0; in bitmap_and() 296 return __bitmap_and(dst, src1, src2, nbits); in bitmap_and() 299 static inline void bitmap_or(unsigned long *dst, const unsigned long *src1, in bitmap_or() argument 303 *dst = *src1 | *src2; in bitmap_or() 305 __bitmap_or(dst, src1, src2, nbits); in bitmap_or() 308 static inline void bitmap_xor(unsigned long *dst, const unsigned long *src1, in bitmap_xor() argument 312 *dst = *src1 ^ *src2; in bitmap_xor() 314 __bitmap_xor(dst, src1, src2, nbits); in bitmap_xor() [all …]
|
| H A D | linkmode.h | 35 static inline int linkmode_andnot(unsigned long *dst, const unsigned long *src1, in linkmode_andnot() argument 38 return bitmap_andnot(dst, src1, src2, __ETHTOOL_LINK_MODE_MASK_NBITS); in linkmode_andnot() 79 static inline int linkmode_equal(const unsigned long *src1, in linkmode_equal() argument 82 return bitmap_equal(src1, src2, __ETHTOOL_LINK_MODE_MASK_NBITS); in linkmode_equal() 85 static inline int linkmode_intersects(const unsigned long *src1, in linkmode_intersects() argument 88 return bitmap_intersects(src1, src2, __ETHTOOL_LINK_MODE_MASK_NBITS); in linkmode_intersects() 91 static inline int linkmode_subset(const unsigned long *src1, in linkmode_subset() argument 94 return bitmap_subset(src1, src2, __ETHTOOL_LINK_MODE_MASK_NBITS); in linkmode_subset()
|
| /OK3568_Linux_fs/kernel/arch/ia64/lib/ |
| H A D | copy_user.S | 66 #define src1 r24 macro 103 mov src1=src // copy because of rotation 115 EX(.failure_in_pipe1,(p16) ld1 val1[0]=[src1],1) 130 and src2=0x7,src1 // src offset 197 EX(.failure_in_pipe2,(p16) ld1 val1[0]=[src1],1) 212 (p14) sub src1=src1,t2 213 (p15) sub src1=src1,t1 243 EX(3f,(p16) ld8 val1[1]=[src1],8); \ 289 (p14) sub src1=src1,t1 300 sub len1=endsrc,src1,1 [all …]
|
| H A D | memcpy_mck.S | 34 #define src1 r3 macro 146 add src1=8,src0 // 2nd src pointer 158 EK(.ex_handler, (p16) ld8 r38=[src1],16) 163 EK(.ex_handler, (p16) ld8 r36=[src1],16) 173 EX(.ex_hndlr_s, (p7) ld8 t2=[src1],8) 177 EX(.ex_hndlr_s, (p8) ld8 t3=[src1]) 206 add src1 = 3*8, src_pre_mem // first t3 src 224 EK(.ex_handler, (p[D]) ld8 t4 = [src1], 3*8) // M1 234 EK(.ex_handler, (p[D]) ld8 t7 = [src1], 3*8) 239 EK(.ex_handler, (p[D]) ld8 t10 = [src1], 8) [all …]
|
| H A D | copy_page_mck.S | 70 #define src1 r3 macro 125 add src1 = 3*8, in1 // first t3 src 144 (p[D]) ld8 t4 = [src1], 3*8 // M1 154 (p[D]) ld8 t7 = [src1], 3*8 159 (p[D]) ld8 t10 = [src1], 8 164 (p[D]) ld8 t11 = [src1], 3*8 169 (p[D]) ld8 t14 = [src1], 8 174 (p[D]) ld8 t15 = [src1], 4*8 179 (p[D-1])ld8 t3 = [src1], 8
|
| /OK3568_Linux_fs/kernel/arch/arm64/lib/ |
| H A D | memcmp.S | 29 src1 .req x0 label 51 eor tmp1, src1, src2 54 ands tmp1, src1, #7 63 ldr data1, [src1], #8 97 bic src1, src1, #7 99 ldr data1, [src1], #8 129 and tmp1, src1, #7 141 ldrb data1w, [src1], #1 157 ands xzr, src1, #7 160 add src1, src1, tmp3 /*backwards src1 to alignment boundary*/ [all …]
|
| H A D | strcmp.S | 33 src1 .req x0 label 52 eor tmp1, src1, src2 56 ands tmp1, src1, #7 65 ldr data1, [src1], #8 82 bic src1, src1, #7 85 ldr data1, [src1], #8 103 and tmp1, src1, #7 112 ldrb data1w, [src1], #1 127 ands xzr, src1, #7 130 add src1, src1, tmp3 [all …]
|
| H A D | strncmp.S | 33 src1 .req x0 label 57 eor tmp1, src1, src2 61 ands tmp1, src1, #7 77 ldr data1, [src1], #8 118 bic src1, src1, #7 120 ldr data1, [src1], #8 147 and tmp1, src1, #7 160 ldrb data1w, [src1], #1 178 ands xzr, src1, #7 180 add src1, src1, tmp3 /*tmp3 is positive in this branch.*/ [all …]
|
| /OK3568_Linux_fs/kernel/drivers/video/rockchip/rga3/ |
| H A D | rga_policy.c | 137 struct rga_img_info_t *src1) in rga_check_src1() argument 139 if (!rga_check_resolution(&data->input_range, src1->act_w, src1->act_h)) in rga_check_src1() 144 src1->act_w + src1->x_offset, in rga_check_src1() 145 src1->act_h + src1->y_offset)) in rga_check_src1() 148 if (!rga_check_format(data, src1->rd_mode, src1->format, 1)) in rga_check_src1() 151 if (!rga_check_align(data->byte_stride_align, src1->format, src1->vir_w)) in rga_check_src1() 221 struct rga_img_info_t *src1 = &job->rga_command_base.pat; in rga_job_assign() local 277 if (src1->yrgb_addr > 0) { in rga_job_assign() 279 (!(src1->rd_mode & data->win[1].rd_mode)) || in rga_job_assign() 310 if (src1->yrgb_addr > 0) { in rga_job_assign() [all …]
|
| /OK3568_Linux_fs/kernel/tools/include/linux/ |
| H A D | bitmap.h | 76 static inline void bitmap_or(unsigned long *dst, const unsigned long *src1, in bitmap_or() argument 80 *dst = *src1 | *src2; in bitmap_or() 82 __bitmap_or(dst, src1, src2, nbits); in bitmap_or() 154 static inline int bitmap_and(unsigned long *dst, const unsigned long *src1, in bitmap_and() argument 158 return (*dst = *src1 & *src2 & BITMAP_LAST_WORD_MASK(nbits)) != 0; in bitmap_and() 159 return __bitmap_and(dst, src1, src2, nbits); in bitmap_and() 170 static inline int bitmap_equal(const unsigned long *src1, in bitmap_equal() argument 174 return !((*src1 ^ *src2) & BITMAP_LAST_WORD_MASK(nbits)); in bitmap_equal() 177 return !memcmp(src1, src2, nbits / 8); in bitmap_equal() 178 return __bitmap_equal(src1, src2, nbits); in bitmap_equal()
|
| /OK3568_Linux_fs/kernel/arch/arc/kernel/ |
| H A D | disasm.c | 113 state->src1 = state->words[1]; in disasm_instr() 115 state->src1 = get_reg(state->wb_reg, regs, cregs); in disasm_instr() 129 state->src1 = FIELD_C(state->words[0]); in disasm_instr() 130 if (state->src1 == REG_LIMM) { in disasm_instr() 132 state->src1 = state->words[1]; in disasm_instr() 134 state->src1 = get_reg(state->src1, regs, cregs); in disasm_instr() 219 state->src1 = state->words[1]; in disasm_instr() 221 state->src1 = get_reg(state->wb_reg, regs, in disasm_instr() 285 state->src1 = get_reg(FIELD_S_B(state->words[0]), regs, cregs); in disasm_instr() 328 state->src1 = get_reg(FIELD_S_B(state->words[0]), regs, cregs); in disasm_instr() [all …]
|
| /OK3568_Linux_fs/kernel/arch/m68k/math-emu/ |
| H A D | multi_arith.h | 114 static inline void fp_submant(struct fp_ext *dest, struct fp_ext *src1, in fp_submant() argument 119 : "g,d" (src2->lowmant), "0,0" (src1->lowmant)); in fp_submant() 121 : "d" (src2->mant.m32[1]), "0" (src1->mant.m32[1])); in fp_submant() 123 : "d" (src2->mant.m32[0]), "0" (src1->mant.m32[0])); in fp_submant() 126 #define fp_mul64(desth, destl, src1, src2) ({ \ argument 128 : "dm" (src1), "0" (src2)); \ 133 #define fp_add64(dest1, dest2, src1, src2) ({ \ argument 137 : "d" (src1), "0" (dest1)); \ 165 static inline void fp_multiplymant(union fp_mant128 *dest, struct fp_ext *src1, in fp_multiplymant() argument 170 fp_mul64(dest->m32[0], dest->m32[1], src1->mant.m32[0], src2->mant.m32[0]); in fp_multiplymant() [all …]
|
| /OK3568_Linux_fs/external/linux-rga/core/ |
| H A D | NormalRga.cpp | 368 int RgaBlit(rga_info *src, rga_info *dst, rga_info *src1) { in RgaBlit() argument 418 if (!src && !dst && !src1) { in RgaBlit() 419 ALOGE("src = %p, dst = %p, src1 = %p", src, dst, src1); in RgaBlit() 442 if (src1) in RgaBlit() 443 memcpy(&relSrc1Rect, &src1->rect, sizeof(rga_rect_t)); in RgaBlit() 449 … (unsigned long)src->hnd, (unsigned long)dst->hnd, (unsigned long)(src1 ? src1->hnd : 0)); in RgaBlit() 451 if (src1) in RgaBlit() 452 …ndle = %d, Fd = %.2d , phyAddr = %p , virAddr = %p\n", src1->handle, src1->fd, src1->phyAddr, src1… in RgaBlit() 456 if (src1) { in RgaBlit() 457 if (src->handle > 0 && dst->handle > 0 && src1->handle > 0) { in RgaBlit() [all …]
|
| /OK3568_Linux_fs/kernel/drivers/video/rockchip/rga2/ |
| H A D | rga2_mmu_info.c | 373 struct rga_img_info_t *src0, *src1, *dst, *els; in rga2_get_dma_info() local 386 src1 = &req->src1; in rga2_get_dma_info() 415 if (unlikely(!mmu_flag && src1->yrgb_addr)) { in rga2_get_dma_info() 419 } else if (mmu_flag && src1->yrgb_addr) { in rga2_get_dma_info() 420 ret = rga2_map_dma_buffer(src1->yrgb_addr, buffer_src1, DMA_BIDIRECTIONAL); in rga2_get_dma_info() 428 ret = rga2_dma_memory_check(buffer_src1, src1); in rga2_get_dma_info() 435 rga2_convert_addr(src1); in rga2_get_dma_info() 607 if ((int)req->src1.yrgb_addr > 0) { in rga2_get_dma_info() 609 req->src1.yrgb_addr); in rga2_get_dma_info() 618 req->src1.yrgb_addr = req->src1.uv_addr; in rga2_get_dma_info() [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/ |
| H A D | core.hpp | 365 CV_EXPORTS_W void add(InputArray src1, InputArray src2, OutputArray dst, 405 CV_EXPORTS_W void subtract(InputArray src1, InputArray src2, OutputArray dst, 430 CV_EXPORTS_W void multiply(InputArray src1, InputArray src2, 453 CV_EXPORTS_W void divide(InputArray src1, InputArray src2, OutputArray dst, 478 CV_EXPORTS_W void scaleAdd(InputArray src1, double alpha, InputArray src2, OutputArray dst); 506 CV_EXPORTS_W void addWeighted(InputArray src1, double alpha, InputArray src2, 683 CV_EXPORTS_W double norm(InputArray src1, int normType = NORM_L2, InputArray mask = noArray()); 696 CV_EXPORTS_W double norm(InputArray src1, InputArray src2, 720 CV_EXPORTS_W double PSNR(InputArray src1, InputArray src2); 727 CV_EXPORTS_W void batchDistance(InputArray src1, InputArray src2, [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/ |
| H A D | core.hpp | 365 CV_EXPORTS_W void add(InputArray src1, InputArray src2, OutputArray dst, 405 CV_EXPORTS_W void subtract(InputArray src1, InputArray src2, OutputArray dst, 430 CV_EXPORTS_W void multiply(InputArray src1, InputArray src2, 453 CV_EXPORTS_W void divide(InputArray src1, InputArray src2, OutputArray dst, 478 CV_EXPORTS_W void scaleAdd(InputArray src1, double alpha, InputArray src2, OutputArray dst); 506 CV_EXPORTS_W void addWeighted(InputArray src1, double alpha, InputArray src2, 683 CV_EXPORTS_W double norm(InputArray src1, int normType = NORM_L2, InputArray mask = noArray()); 696 CV_EXPORTS_W double norm(InputArray src1, InputArray src2, 720 CV_EXPORTS_W double PSNR(InputArray src1, InputArray src2); 727 CV_EXPORTS_W void batchDistance(InputArray src1, InputArray src2, [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/ |
| H A D | core.hpp | 365 CV_EXPORTS_W void add(InputArray src1, InputArray src2, OutputArray dst, 405 CV_EXPORTS_W void subtract(InputArray src1, InputArray src2, OutputArray dst, 430 CV_EXPORTS_W void multiply(InputArray src1, InputArray src2, 453 CV_EXPORTS_W void divide(InputArray src1, InputArray src2, OutputArray dst, 478 CV_EXPORTS_W void scaleAdd(InputArray src1, double alpha, InputArray src2, OutputArray dst); 506 CV_EXPORTS_W void addWeighted(InputArray src1, double alpha, InputArray src2, 683 CV_EXPORTS_W double norm(InputArray src1, int normType = NORM_L2, InputArray mask = noArray()); 696 CV_EXPORTS_W double norm(InputArray src1, InputArray src2, 720 CV_EXPORTS_W double PSNR(InputArray src1, InputArray src2); 727 CV_EXPORTS_W void batchDistance(InputArray src1, InputArray src2, [all …]
|