Searched refs:imm (Results 1 - 25 of 93) sorted by relevance

1234

/freebsd-11-stable/contrib/llvm-project/clang/lib/Headers/
H A Df16cintrin.h52 /// unsigned short _cvtss_sh(float a, const int imm);
60 /// \param imm
68 #define _cvtss_sh(a, imm) \
70 (imm)))[0])
78 /// __m128i _mm_cvtps_ph(__m128 a, const int imm);
85 /// \param imm
95 #define _mm_cvtps_ph(a, imm) \
96 (__m128i)__builtin_ia32_vcvtps2ph((__v4sf)(__m128)(a), (imm))
121 /// __m128i _mm256_cvtps_ph(__m256 a, const int imm);
129 /// \param imm
[all...]
H A Drtmintrin.h41 #define _xabort(imm) __builtin_ia32_xabort((imm))
H A Davx512dqintrin.h1220 #define _mm512_extractf32x8_ps(A, imm) \
1221 (__m256)__builtin_ia32_extractf32x8_mask((__v16sf)(__m512)(A), (int)(imm), \
1225 #define _mm512_mask_extractf32x8_ps(W, U, A, imm) \
1226 (__m256)__builtin_ia32_extractf32x8_mask((__v16sf)(__m512)(A), (int)(imm), \
1230 #define _mm512_maskz_extractf32x8_ps(U, A, imm) \
1231 (__m256)__builtin_ia32_extractf32x8_mask((__v16sf)(__m512)(A), (int)(imm), \
1235 #define _mm512_extractf64x2_pd(A, imm) \
1237 (int)(imm), \
1241 #define _mm512_mask_extractf64x2_pd(W, U, A, imm) \
1243 (int)(imm), \
[all...]
H A Davx512vldqintrin.h1068 #define _mm256_extractf64x2_pd(A, imm) \
1070 (int)(imm), \
1074 #define _mm256_mask_extractf64x2_pd(W, U, A, imm) \
1076 (int)(imm), \
1080 #define _mm256_maskz_extractf64x2_pd(U, A, imm) \
1082 (int)(imm), \
1086 #define _mm256_extracti64x2_epi64(A, imm) \
1088 (int)(imm), \
1092 #define _mm256_mask_extracti64x2_epi64(W, U, A, imm) \
1094 (int)(imm), \
[all...]
/freebsd-11-stable/sys/riscv/riscv/
H A Ddb_disasm.c53 int funct7; /* Or imm, depending on type. */
196 int imm; member in struct:csr_op
280 int imm; local
282 imm = 0;
285 imm = i.IType.imm;
286 *val = imm;
287 if (imm & (1 << 11))
288 imm |= (0xfffff << 12); /* sign extend */
291 imm
324 oprint(struct riscv_op *op, vm_offset_t loc, int rd, int rs1, int rs2, uint32_t val, vm_offset_t imm) argument
397 int imm; local
[all...]
/freebsd-11-stable/contrib/gcc/
H A Dtree-ssanames.c124 use_operand_p imm; local
160 imm = &(SSA_NAME_IMM_USE_NODE (t));
161 imm->use = NULL;
162 imm->prev = imm;
163 imm->next = imm;
164 imm->stmt = t;
208 use_operand_p imm = &(SSA_NAME_IMM_USE_NODE (var)); local
213 while (imm
[all...]
H A Dtree-phinodes.c229 use_operand_p imm; local
230 imm = &(PHI_ARG_IMM_USE_NODE (phi, i));
231 imm->use = &(PHI_ARG_DEF_TREE (phi, i));
232 imm->prev = NULL;
233 imm->next = NULL;
234 imm->stmt = phi;
250 use_operand_p imm; local
251 imm = &(PHI_ARG_IMM_USE_NODE (phi, x));
252 delink_imm_use (imm);
285 use_operand_p imm, old_im local
296 use_operand_p imm; local
[all...]
H A Dtree-flow-inline.h402 end_readonly_imm_use_p (imm_use_iterator *imm) argument
404 return (imm->imm_use == imm->end_p);
409 first_readonly_imm_use (imm_use_iterator *imm, tree var) argument
413 imm->end_p = &(SSA_NAME_IMM_USE_NODE (var));
414 imm->imm_use = imm->end_p->next;
416 imm->iter_node.next = imm->imm_use->next;
418 if (end_readonly_imm_use_p (imm))
425 next_readonly_imm_use(imm_use_iterator *imm) argument
1307 end_imm_use_stmt_p(imm_use_iterator *imm) argument
1316 end_imm_use_stmt_traverse(imm_use_iterator *imm) argument
1354 link_use_stmts_after(use_operand_p head, imm_use_iterator *imm) argument
1386 first_imm_use_stmt(imm_use_iterator *imm, tree var) argument
1413 next_imm_use_stmt(imm_use_iterator *imm) argument
1432 first_imm_use_on_stmt(imm_use_iterator *imm) argument
1441 end_imm_use_on_stmt_p(imm_use_iterator *imm) argument
1449 next_imm_use_on_stmt(imm_use_iterator *imm) argument
[all...]
/freebsd-11-stable/contrib/llvm-project/llvm/lib/Target/Sparc/
H A DSparc.h149 inline static unsigned HI22(int64_t imm) { argument
150 return (unsigned)((imm >> 10) & ((1 << 22)-1));
153 inline static unsigned LO10(int64_t imm) { argument
154 return (unsigned)(imm & 0x3FF);
157 inline static unsigned HIX22(int64_t imm) { argument
158 return HI22(~imm);
161 inline static unsigned LOX10(int64_t imm) { argument
162 return ~LO10(~imm);
/freebsd-11-stable/contrib/llvm-project/llvm/lib/Target/VE/
H A DVE.h100 inline static int64_t HI32(int64_t imm) { argument
101 return (int32_t)(imm >> 32);
104 inline static int64_t LO32(int64_t imm) { argument
105 return (int32_t)(imm);
/freebsd-11-stable/contrib/binutils/opcodes/
H A Dsh-dis.c498 int imm = 0; local
527 imm = (nibs[2] << 4) | (nibs[3]);
528 if (imm & 0x80)
529 imm |= ~0xff;
530 imm = ((char) imm) * 2 + 4;
533 imm = ((nibs[1]) << 8) | (nibs[2] << 4) | (nibs[3]);
534 if (imm & 0x800)
535 imm |= ~0xfff;
536 imm
[all...]
H A Dsparc-dis.c668 int imm; local
671 imm = X_SIMM (insn, 13);
673 imm = X_SIMM (insn, 11);
675 imm = X_SIMM (insn, 10);
687 if (imm <= 9)
688 (*info->fprintf_func) (stream, "%d", imm);
690 (*info->fprintf_func) (stream, "%#x", imm);
697 int imm = X_IMM (insn, *s == 'X' ? 5 : 6); local
699 if (imm <= 9)
700 (info->fprintf_func) (stream, "%d", imm);
[all...]
H A Darm-dis.c1765 int imm;
1767 imm = (given & 0xf) | ((given & 0xe0) >> 1);
1769 /* Is ``imm'' a negative number? */
1770 if (imm & 0x40)
1771 imm |= -(1 << 7);
1773 func (stream, "%d", imm);
2977 int imm;
2979 imm = (given & 0xf) | ((given & 0xfff00) >> 4);
2980 func (stream, "%d", imm);
3171 long imm
1764 int imm; local
2976 int imm; local
3170 long imm = (given & 0x07c0) >> 6; local
3360 unsigned int bits = 0, imm, imm8, mod; local
3383 unsigned int imm = 0; local
3394 unsigned int imm = 0; local
3406 unsigned int imm = 0; local
[all...]
/freebsd-11-stable/sys/arm64/arm64/
H A Ddisassem.c85 TYPE_01, /* OP <RD>, <RN>, <RM>{, <shift [LSL, LSR, ASR]> #<imm>} SF32/64
86 OP <RD>, <RN>, #<imm>{, <shift [0, 12]>} SF32/64 */
87 TYPE_02, /* OP <RT>, [<RN>, #<imm>]{!}] SF32/64
88 OP <RT>, [<RN>], #<imm>{!} SF32/64
90 TYPE_03, /* OP <RT>, #imm SF32/64 */
342 int shift, rm, rt, rd, rn, imm, sf, idx, option, scale, amount; local
351 shift = rd = rm = rn = imm = idx = option = amount = scale = 0;
382 arm64_disasm_read_token_sign_ext(i_ptr, insn, "IMM", &imm);
384 arm64_disasm_read_token(i_ptr, insn, "IMM", &imm);
386 imm <<
[all...]
/freebsd-11-stable/sys/mips/mips/
H A Ddb_trace.c297 args[0] = kdbpeek((int *)(sp + (short)i.IType.imm));
302 args[1] = kdbpeek((int *)(sp + (short)i.IType.imm));
307 args[2] = kdbpeek((int *)(sp + (short)i.IType.imm));
312 args[3] = kdbpeek((int *)(sp + (short)i.IType.imm));
317 ra = kdbpeek((int *)(sp + (short)i.IType.imm));
331 args[0] = kdbpeekd((int *)(sp + (short)i.IType.imm));
336 args[1] = kdbpeekd((int *)(sp + (short)i.IType.imm));
341 args[2] = kdbpeekd((int *)(sp + (short)i.IType.imm));
346 args[3] = kdbpeekd((int *)(sp + (short)i.IType.imm));
351 ra = kdbpeekd((int *)(sp + (short)i.IType.imm));
[all...]
H A Ddb_disasm.c258 db_printf("0x%08x", mdbdot + 4 + ((short)i.IType.imm << 2));
355 db_printf("%d(%s)", (short)i.IType.imm, reg_name[i.IType.rs]);
362 reg_name[i.IType.rt], i.IType.imm);
368 reg_name[i.IType.rt], reg_name[i.IType.rs], i.IType.imm);
373 reg_name[i.IType.rt], i.IType.imm);
382 (short)i.IType.imm);
389 (short)i.IType.imm);
H A Dstack_machdep.c72 stacksize = -(short)insn.IType.imm;
79 ra_stack_pos = (short)insn.IType.imm;
/freebsd-11-stable/crypto/openssl/crypto/perlasm/
H A Dx86asm.pl87 { my($dst,$src,$imm)=@_;
89 { &::data_byte(0x66,0x0f,0x3a,0x16,0xc0|($2<<3)|$regrm{$1},$imm); }
95 { my($dst,$src,$imm)=@_;
97 { &::data_byte(0x66,0x0f,0x3a,0x22,0xc0|($1<<3)|$regrm{$2},$imm); }
111 { my($dst,$src,$imm)=@_;
113 { &::data_byte(0x66,0x0f,0x3a,0x0f,0xc0|($1<<3)|$2,$imm); }
119 { my($dst,$src,$imm)=@_;
121 { &::data_byte(0x66,0x0f,0x3a,0x44,0xc0|($1<<3)|$2,$imm); }
/freebsd-11-stable/sys/riscv/include/
H A Driscv_opcode.h75 unsigned imm: 12; member in struct:__anon13242::__anon13245
/freebsd-11-stable/sys/cddl/dev/dtrace/riscv/
H A Ddtrace_subr.c246 uint32_t imm; local
260 imm = i.SType.imm0_4 | (i.SType.imm5_11 << 5);
261 sp = (register_t *)((uint8_t *)frame->tf_sp + imm);
/freebsd-11-stable/contrib/llvm-project/llvm/lib/Target/ARM/Disassembler/
H A DARMDisassembler.cpp1455 unsigned imm = fieldFromInstruction(Val, 7, 5); local
1477 if (Shift == ARM_AM::ror && imm == 0)
1480 unsigned Op = Shift | (imm << 3);
1651 unsigned imm = fieldFromInstruction(Insn, 0, 8); local
1767 imm = ARM_AM::getAM5Opc(U ? ARM_AM::add : ARM_AM::sub, imm);
1768 Inst.addOperand(MCOperand::createImm(imm));
1786 imm |= U << 8;
1791 Inst.addOperand(MCOperand::createImm(imm));
1830 unsigned imm local
1913 unsigned imm = ARM_AM::getAM2Opc(Op, amt, Opc, idx_mode); local
1935 unsigned imm = fieldFromInstruction(Val, 7, 5); local
1980 unsigned imm = fieldFromInstruction(Insn, 8, 4); local
2408 int imm = fieldFromInstruction(Insn, 0, 8); local
2423 unsigned imm = 0; local
2448 unsigned imm = 0; local
2551 unsigned imm = fieldFromInstruction(Val, 0, 12); local
2573 unsigned imm = fieldFromInstruction(Val, 0, 8); local
2593 unsigned imm = fieldFromInstruction(Val, 0, 8); local
2644 unsigned imm = fieldFromInstruction(Insn, 0, 24) << 2; local
3467 unsigned imm = fieldFromInstruction(Insn, 0, 4); local
3514 unsigned imm = fieldFromInstruction(Insn, 0, 4); local
3644 unsigned imm = fieldFromInstruction(Insn, 0, 8); local
3707 unsigned imm = fieldFromInstruction(Val, 3, 5); local
3718 unsigned imm = Val << 2; local
3740 unsigned imm = fieldFromInstruction(Val, 0, 2); local
3853 unsigned imm = fieldFromInstruction(Insn, 0, 8); local
3936 unsigned imm = fieldFromInstruction(Insn, 0, 12); local
4016 unsigned imm = fieldFromInstruction(Insn, 0, 8); local
4055 int imm = fieldFromInstruction(Insn, 0, 12); local
4107 int imm = Val & 0xFF; local
4121 int imm = Val & 0x7F; local
4136 unsigned imm = fieldFromInstruction(Val, 0, 9); local
4152 unsigned imm = fieldFromInstruction(Val, 0, 8); local
4167 unsigned imm = fieldFromInstruction(Val, 0, 8); local
4179 int imm = Val & 0xFF; local
4192 int imm = Val & 0x7F; local
4209 unsigned imm = fieldFromInstruction(Val, 0, 9); local
4257 unsigned imm = fieldFromInstruction(Val, 0, 8); local
4274 unsigned imm = fieldFromInstruction(Val, 0, 8); local
4352 unsigned imm = fieldFromInstruction(Val, 0, 12); local
4375 unsigned imm = fieldFromInstruction(Insn, 0, 7); local
4452 int imm = fieldFromInstruction(Insn, 0, 7); local
4547 unsigned imm = fieldFromInstruction(Insn, 0, 4); local
4573 unsigned imm = fieldFromInstruction(Val, 0, 8); local
4592 unsigned imm = (unrot >> rot) | (unrot << ((32-rot)&31)); local
4800 unsigned imm = fieldFromInstruction(Insn, 0, 12); local
4825 unsigned imm = fieldFromInstruction(Insn, 0, 12); local
4852 unsigned imm = fieldFromInstruction(Insn, 0, 12); local
4877 unsigned imm = fieldFromInstruction(Insn, 0, 12); local
5671 unsigned imm = fieldFromInstruction(Insn, 16, 6); local
5730 unsigned imm = fieldFromInstruction(Insn, 16, 6); local
[all...]
/freebsd-11-stable/contrib/ofed/libmlx4/
H A Dwqe.h85 * imm is immediate data for send/RDMA write w/ immediate;
89 uint32_t imm; member in struct:mlx4_wqe_ctrl_seg
/freebsd-11-stable/sys/dev/mthca/
H A Dmthca_wqe.h61 __be32 imm; /* immediate data */ member in struct:mthca_next_seg
/freebsd-11-stable/contrib/llvm-project/lld/ELF/Arch/
H A DRISCV.cpp64 static uint32_t itype(uint32_t op, uint32_t rd, uint32_t rs1, uint32_t imm) { argument
65 return op | (rd << 7) | (rs1 << 15) | (imm << 20);
70 static uint32_t utype(uint32_t op, uint32_t rd, uint32_t imm) { argument
71 return op | (rd << 7) | (imm << 12);
306 int64_t imm = SignExtend64(val + 0x800, bits) >> 12; local
307 checkInt(loc, imm, 6, type);
308 if (imm == 0) { // `c.lui rd, 0` is illegal, convert to `c.li rd, 0`
/freebsd-11-stable/contrib/llvm-project/llvm/lib/ExecutionEngine/RuntimeDyld/Targets/
H A DRuntimeDyldCOFFAArch64.h37 static void write32AArch64Imm(uint8_t *T, uint64_t imm, uint32_t rangeLimit) { argument
40 write32le(T, orig | ((imm & (0xFFF >> rangeLimit)) << 10));
43 static void write32AArch64Ldr(uint8_t *T, uint64_t imm) { argument
50 if ((imm & ((1 << size) - 1)) != 0)
52 write32AArch64Imm(T, imm >> size, size);

Completed in 413 milliseconds

1234