Home
last modified time | relevance | path

Searched refs:IMM_L (Results 1 – 9 of 9) sorted by relevance

/OK3568_Linux_fs/kernel/arch/powerpc/include/asm/
H A Dppc-opcode.h79 #define IMM_L(i) ((uintptr_t)(i) & 0xffff) macro
419 #define PPC_RAW_LWZ(r, base, i) (0x80000000 | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
439 #define PPC_RAW_ADDI(d, a, i) (PPC_INST_ADDI | ___PPC_RT(d) | ___PPC_RA(a) | IMM_L(i))
441 #define PPC_RAW_ADDIS(d, a, i) (PPC_INST_ADDIS | ___PPC_RT(d) | ___PPC_RA(a) | IMM_L(i))
445 #define PPC_RAW_STW(r, base, i) (0x90000000 | ___PPC_RS(r) | ___PPC_RA(base) | IMM_L(i))
446 #define PPC_RAW_STWU(r, base, i) (0x94000000 | ___PPC_RS(r) | ___PPC_RA(base) | IMM_L(i))
447 #define PPC_RAW_STH(r, base, i) (0xb0000000 | ___PPC_RS(r) | ___PPC_RA(base) | IMM_L(i))
448 #define PPC_RAW_STB(r, base, i) (0x98000000 | ___PPC_RS(r) | ___PPC_RA(base) | IMM_L(i))
449 #define PPC_RAW_LBZ(r, base, i) (0x88000000 | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
451 #define PPC_RAW_LHZ(r, base, i) (0xa0000000 | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
[all …]
/OK3568_Linux_fs/kernel/arch/powerpc/net/
H A Dbpf_jit32.h77 EMIT(PPC_RAW_LBZ(r, r, IMM_L(i))); } } while(0)
81 EMIT(PPC_RAW_LD(r, r, IMM_L(i))); } } while(0)
85 EMIT(PPC_RAW_LWZ(r, r, IMM_L(i))); } } while(0)
89 EMIT(PPC_RAW_LHZ(r, r, IMM_L(i))); } } while(0)
H A Dbpf_jit_comp.c142 EMIT(PPC_RAW_ADDI(r_A, r_A, IMM_L(K))); in bpf_jit_build_body()
153 EMIT(PPC_RAW_ADDI(r_A, r_A, IMM_L(-K))); in bpf_jit_build_body()
217 if (IMM_L(K)) in bpf_jit_build_body()
218 EMIT(PPC_RAW_ORI(r_A, r_A, IMM_L(K))); in bpf_jit_build_body()
228 if (IMM_L(K)) in bpf_jit_build_body()
229 EMIT(PPC_RAW_XORI(r_A, r_A, IMM_L(K))); in bpf_jit_build_body()
444 EMIT(PPC_RAW_ADDI(r_addr, r_X, IMM_L(K))); in bpf_jit_build_body()
H A Dbpf_jit.h55 if (IMM_L(i)) \
56 EMIT(PPC_RAW_ORI(d, d, IMM_L(i))); \
H A Dbpf_jit_comp64.c380 EMIT(PPC_RAW_ADDI(dst_reg, dst_reg, IMM_L(imm))); in bpf_jit_build_body()
391 EMIT(PPC_RAW_ADDI(dst_reg, dst_reg, IMM_L(-imm))); in bpf_jit_build_body()
407 EMIT(PPC_RAW_MULI(dst_reg, dst_reg, IMM_L(imm))); in bpf_jit_build_body()
500 EMIT(PPC_RAW_ANDI(dst_reg, dst_reg, IMM_L(imm))); in bpf_jit_build_body()
518 if (IMM_L(imm)) in bpf_jit_build_body()
519 EMIT(PPC_RAW_ORI(dst_reg, dst_reg, IMM_L(imm))); in bpf_jit_build_body()
535 if (IMM_L(imm)) in bpf_jit_build_body()
536 EMIT(PPC_RAW_XORI(dst_reg, dst_reg, IMM_L(imm))); in bpf_jit_build_body()
/OK3568_Linux_fs/kernel/arch/powerpc/lib/
H A Dtest_emulate_step.c26 PPC_INST_PLD | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
34 PPC_INST_PSTD | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
38 PPC_INST_LFS | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
42 PPC_INST_STFS | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
46 PPC_INST_LFD | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
50 PPC_INST_STFD | ___PPC_RT(r) | ___PPC_RA(base) | IMM_L(i))
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/hal/
H A Dintrin_avx.hpp951 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_right() enumerator
960 return v_uint8x32(_mm256_alignr_epi8(b.val, swap, IMM_L)); in v_rotate_right()
966 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_left() enumerator
976 return v_uint8x32(_mm256_slli_si256(swapz, IMM_L)); in v_rotate_left()
982 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_right() enumerator
991 return v_uint8x32(_mm256_srli_si256(swapz, IMM_L)); in v_rotate_right()
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/hal/
H A Dintrin_avx.hpp951 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_right() enumerator
960 return v_uint8x32(_mm256_alignr_epi8(b.val, swap, IMM_L)); in v_rotate_right()
966 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_left() enumerator
976 return v_uint8x32(_mm256_slli_si256(swapz, IMM_L)); in v_rotate_left()
982 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_right() enumerator
991 return v_uint8x32(_mm256_srli_si256(swapz, IMM_L)); in v_rotate_right()
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/hal/
H A Dintrin_avx.hpp951 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_right() enumerator
960 return v_uint8x32(_mm256_alignr_epi8(b.val, swap, IMM_L)); in v_rotate_right()
966 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_left() enumerator
976 return v_uint8x32(_mm256_slli_si256(swapz, IMM_L)); in v_rotate_left()
982 enum {IMM_L = (imm - 16) & 0xFF}; in v_rotate_right() enumerator
991 return v_uint8x32(_mm256_srli_si256(swapz, IMM_L)); in v_rotate_right()