| /src/sys/arch/x68k/stand/libiocs/ |
| iocscall.h | 11 # define IMM \#
13 # define IMM #
17 moveq IMM n,%d0;\
18 trap IMM 15
41 moveq IMM s,%d1;\
|
| /src/sys/external/bsd/sljit/dist/sljit_src/ |
| sljitNativeMIPS_64.c | 31 static sljit_s32 load_immediate(struct sljit_compiler *compiler, sljit_s32 dst_ar, sljit_sw imm)
39 if (!(imm & ~0xffff))
40 return push_inst(compiler, ORI | SA(0) | TA(dst_ar) | IMM(imm), dst_ar);
42 if (imm < 0 && imm >= SIMM_MIN)
43 return push_inst(compiler, ADDIU | SA(0) | TA(dst_ar) | IMM(imm), dst_ar);
45 if (imm <= 0x7fffffffl && imm >= -0x80000000l)
[all...] |
| sljitNativeSPARC_32.c | 29 static sljit_s32 load_immediate(struct sljit_compiler *compiler, sljit_s32 dst, sljit_sw imm)
31 if (imm <= SIMM_MAX && imm >= SIMM_MIN)
32 return push_inst(compiler, OR | D(dst) | S1(0) | IMM(imm), DR(dst));
34 FAIL_IF(push_inst(compiler, SETHI | D(dst) | ((imm >> 10) & 0x3fffff), DR(dst)));
35 return (imm & 0x3ff) ? push_inst(compiler, OR | D(dst) | S1(dst) | IMM_ARG | (imm & 0x3ff), DR(dst)) : SLJIT_SUCCESS;
38 #define ARG2(flags, src2) ((flags & SRC2_IMM) ? IMM(src2) : S2(src2))
60 return push_inst(compiler, AND | D(dst) | S1(src2) | IMM(0xff), DR(dst))
[all...] |
| sljitNativePPC_64.c | 46 static sljit_s32 load_immediate(struct sljit_compiler *compiler, sljit_s32 reg, sljit_sw imm)
53 if (imm <= SIMM_MAX && imm >= SIMM_MIN)
54 return push_inst(compiler, ADDI | D(reg) | A(0) | IMM(imm));
56 if (!(imm & ~0xffff))
57 return push_inst(compiler, ORI | S(TMP_ZERO) | A(reg) | IMM(imm));
59 if (imm <= 0x7fffffffl && imm >= -0x80000000l)
[all...] |
| sljitNativeMIPS_32.c | 31 static sljit_s32 load_immediate(struct sljit_compiler *compiler, sljit_s32 dst_ar, sljit_sw imm)
33 if (!(imm & ~0xffff))
34 return push_inst(compiler, ORI | SA(0) | TA(dst_ar) | IMM(imm), dst_ar);
36 if (imm < 0 && imm >= SIMM_MIN)
37 return push_inst(compiler, ADDIU | SA(0) | TA(dst_ar) | IMM(imm), dst_ar);
39 FAIL_IF(push_inst(compiler, LUI | TA(dst_ar) | IMM(imm >> 16), dst_ar))
[all...] |
| sljitNativePPC_32.c | 31 static sljit_s32 load_immediate(struct sljit_compiler *compiler, sljit_s32 reg, sljit_sw imm)
33 if (imm <= SIMM_MAX && imm >= SIMM_MIN)
34 return push_inst(compiler, ADDI | D(reg) | A(0) | IMM(imm));
36 if (!(imm & ~0xffff))
37 return push_inst(compiler, ORI | S(TMP_ZERO) | A(reg) | IMM(imm));
39 FAIL_IF(push_inst(compiler, ADDIS | D(reg) | A(0) | IMM(imm >> 16)))
[all...] |
| sljitNativeMIPS_common.c | 86 #define IMM(imm) ((imm) & 0xffff)
87 #define SH_IMM(imm) ((imm) << 6)
564 FAIL_IF(push_inst(compiler, ADDIU_W | S(SLJIT_SP) | T(SLJIT_SP) | IMM(-local_size), DR(SLJIT_SP)));
576 FAIL_IF(push_inst(compiler, STACK_STORE | base | TA(RETURN_ADDR_REG) | IMM(offs), MOVABLE_INS));
581 FAIL_IF(push_inst(compiler, STACK_STORE | base | T(i) | IMM(offs), MOVABLE_INS));
586 FAIL_IF(push_inst(compiler, STACK_STORE | base | T(i) | IMM(offs), MOVABLE_INS));
636 FAIL_IF(push_inst(compiler, STACK_LOAD | base | TA(RETURN_ADDR_REG) | IMM(local_size - (sljit_s32)sizeof(sljit_sw)), RETURN_ADDR_REG))
[all...] |
| sljitNativeSPARC_common.c | 116 #define IMM(imm) (((imm) & 0x1fff) | IMM_ARG)
450 FAIL_IF(push_inst(compiler, SAVE | D(SLJIT_SP) | S1(SLJIT_SP) | IMM(-local_size), UNMOVABLE_INS));
484 FAIL_IF(push_inst(compiler, JMPL | D(0) | S1A(31) | IMM(8), UNMOVABLE_INS));
538 | S1(arg & REG_MASK) | ((arg & OFFS_REG_MASK) ? S2(OFFS_REG(arg)) : IMM(argw)),
604 FAIL_IF(push_inst(compiler, ADD | D(TMP_REG3) | S1(TMP_REG3) | IMM(argw - compiler->cache_argw), DR(TMP_REG3)));
625 return push_inst(compiler, data_transfer_insts[flags & MEM_MASK] | dest | S1(arg2) | IMM(0), delay_slot);
654 arg2 goes to TMP_REG2, imm or src reg
805 FAIL_IF(push_inst(compiler, SRA | D(TMP_REG1) | S1(SLJIT_R0) | IMM(31), DR(TMP_REG1)))
[all...] |
| sljitNativePPC_common.c | 127 #define IMM(imm) ((imm) & 0xffff)
607 FAIL_IF(push_inst(compiler, STACK_STORE | S(TMP_ZERO) | A(SLJIT_SP) | IMM(offs)));
612 FAIL_IF(push_inst(compiler, STACK_STORE | S(i) | A(SLJIT_SP) | IMM(offs)));
617 FAIL_IF(push_inst(compiler, STACK_STORE | S(i) | A(SLJIT_SP) | IMM(offs)));
623 FAIL_IF(push_inst(compiler, STACK_STORE | S(0) | A(SLJIT_SP) | IMM(2 * sizeof(sljit_sw))));
625 FAIL_IF(push_inst(compiler, STACK_STORE | S(0) | A(SLJIT_SP) | IMM(sizeof(sljit_sw))));
642 FAIL_IF(push_inst(compiler, STWU | S(SLJIT_SP) | A(SLJIT_SP) | IMM(-local_size)));
649 FAIL_IF(push_inst(compiler, STDU | S(SLJIT_SP) | A(SLJIT_SP) | IMM(-local_size)))
[all...] |
| /src/sys/external/bsd/compiler_rt/dist/lib/builtins/arm/ |
| udivmodsi4.S | 119 #define IMM #
122 cmp r0, r1, lsl IMM shift; \
124 WIDE(addhs) r3, r3, IMM (1 << shift); \
125 WIDE(subhs) r0, r0, r1, lsl IMM shift
|
| udivsi3.S | 116 #define IMM #
119 cmp r0, r1, lsl IMM shift; \
121 WIDE(addhs) r3, r3, IMM (1 << shift); \
122 WIDE(subhs) r0, r0, r1, lsl IMM shift
|
| umodsi3.S | 110 #define IMM #
113 cmp r0, r1, lsl IMM shift; \
115 WIDE(subhs) r0, r0, r1, lsl IMM shift
|
| /src/sys/external/isc/libsodium/dist/src/libsodium/crypto_stream/chacha20/dolbeau/ |
| u4.h | 2 #define VEC4_ROT(A, IMM) \
3 _mm_or_si128(_mm_slli_epi32(A, IMM), _mm_srli_epi32(A, (32 - IMM)))
|
| u8.h | 2 #define VEC8_ROT(A, IMM) \
3 _mm256_or_si256(_mm256_slli_epi32(A, IMM), _mm256_srli_epi32(A, (32 - IMM)))
|
| /src/sys/arch/powerpc/powerpc/ |
| db_disasm.c | 877 u_int IMM;
879 IMM = extract_field(instr, 31 - 31, 16);
880 if (IMM & 0x8000) {
882 IMM = 0x10000-IMM;
887 IMM = extract_field(instr, 31 - 31, 16);
891 db_printf("0x%x", IMM);
|
