/freebsd-11-stable/contrib/llvm-project/clang/lib/Headers/ |
H A D | f16cintrin.h | 52 /// 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 D | rtmintrin.h | 41 #define _xabort(imm) __builtin_ia32_xabort((imm))
|
H A D | avx512dqintrin.h | 1220 #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 D | avx512vldqintrin.h | 1068 #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 D | db_disasm.c | 53 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 D | tree-ssanames.c | 124 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 D | tree-phinodes.c | 229 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 D | tree-flow-inline.h | 402 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 D | Sparc.h | 149 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 D | VE.h | 100 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 D | sh-dis.c | 498 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 D | sparc-dis.c | 668 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 D | arm-dis.c | 1765 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 D | disassem.c | 85 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 D | db_trace.c | 297 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 D | db_disasm.c | 258 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 D | stack_machdep.c | 72 stacksize = -(short)insn.IType.imm; 79 ra_stack_pos = (short)insn.IType.imm;
|
/freebsd-11-stable/crypto/openssl/crypto/perlasm/ |
H A D | x86asm.pl | 87 { 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 D | riscv_opcode.h | 75 unsigned imm: 12; member in struct:__anon13242::__anon13245
|
/freebsd-11-stable/sys/cddl/dev/dtrace/riscv/ |
H A D | dtrace_subr.c | 246 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 D | ARMDisassembler.cpp | 1455 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 D | wqe.h | 85 * 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 D | mthca_wqe.h | 61 __be32 imm; /* immediate data */ member in struct:mthca_next_seg
|
/freebsd-11-stable/contrib/llvm-project/lld/ELF/Arch/ |
H A D | RISCV.cpp | 64 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 D | RuntimeDyldCOFFAArch64.h | 37 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);
|