Home
last modified time | relevance | path

Searched refs:sljit_u32 (Results 1 – 17 of 17) sorted by relevance

/third_party/pcre2/pcre2/src/sljit/
DsljitNativeMIPS_32.c66 …s(struct sljit_compiler *compiler, sljit_s32 arg_types, sljit_ins *ins_ptr, sljit_u32 *extra_space) in call_with_args()
68 sljit_u32 is_tail_call = *extra_space & SLJIT_CALL_RETURN; in call_with_args()
69 sljit_u32 offset = 0; in call_with_args()
199 sljit_u32 extra_space = 0; in sljit_emit_call()
210 extra_space = (sljit_u32)type; in sljit_emit_call()
255 sljit_u32 extra_space = (sljit_u32)type; in sljit_emit_icall()
DsljitNativeARM_64.c33 typedef sljit_u32 sljit_ins;
242 sljit_u32 dst; in sljit_generate_code()
440 static sljit_ins logical_imm(sljit_sw imm, sljit_u32 len) in logical_imm()
443 sljit_u32 ones, right; in logical_imm()
510 sljit_u32 i, zeros, ones, first; in load_immediate()
901 sljit_u32 shift = MEM_SIZE_SHIFT(flags); in emit_op_mem()
902 sljit_u32 type = (shift << 30); in emit_op_mem()
1373 srcw = (sljit_u32)srcw; in sljit_emit_op1()
1609 void *instruction, sljit_u32 size) in sljit_emit_op_custom()
1624 sljit_u32 shift = MEM_SIZE_SHIFT(flags); in emit_fop_mem()
[all …]
DsljitNativeARM_T2_32.c37 typedef sljit_u32 sljit_ins;
324 …diff = ((sljit_sw)jump->u.target - (sljit_sw)(jump->addr + sizeof(sljit_u32)) - executable_offset)… in set_jump_instruction()
328 …diff = ((sljit_sw)(jump->u.label->addr) - (sljit_sw)(jump->addr + sizeof(sljit_u32)) - executable_… in set_jump_instruction()
1146 sljit_u32 float_arg_count; in sljit_emit_enter()
1148 sljit_u32 old_offset, f32_offset; in sljit_emit_enter()
1149 sljit_u32 remap[3]; in sljit_emit_enter()
1150 sljit_u32 *remap_ptr = remap; in sljit_emit_enter()
1925 void *instruction, sljit_u32 size) in sljit_emit_op_custom()
2306 …_args(struct sljit_compiler *compiler, sljit_s32 arg_types, sljit_s32 *src, sljit_u32 *extra_space) in softfloat_call_with_args()
2308 sljit_u32 is_tail_call = *extra_space & SLJIT_CALL_RETURN; in softfloat_call_with_args()
[all …]
DsljitNativeARM_32.c345 sljit_u32 value; in resolve_const_pool_index()
411 FAIL_IF(push_inst(compiler, MOVW | RD(reg) | ((imm << 4) & 0xf0000) | ((sljit_u32)imm & 0xfff))); in emit_imm()
412 …return push_inst(compiler, MOVT | RD(reg) | ((imm >> 12) & 0xf0000) | (((sljit_u32)imm >> 16) & 0x… in emit_imm()
1067 sljit_u32 float_arg_count; in sljit_emit_enter()
1069 sljit_u32 old_offset, f32_offset; in sljit_emit_enter()
1070 sljit_u32 remap[3]; in sljit_emit_enter()
1071 sljit_u32 *remap_ptr = remap; in sljit_emit_enter()
1623 sljit_u32 rol; in get_imm()
2332 void *instruction, sljit_u32 size) in sljit_emit_op_custom()
2729 …_args(struct sljit_compiler *compiler, sljit_s32 arg_types, sljit_s32 *src, sljit_u32 *extra_space) in softfloat_call_with_args()
[all …]
DsljitNativeX86_common.c304 static sljit_u32 cpu_feature_list = 0;
337 sljit_u32 feature_list = CPU_FEATURE_DETECTED; in get_cpu_features()
338 sljit_u32 value; in get_cpu_features()
356 value = (sljit_u32)CPUInfo[3]; in get_cpu_features()
1657 srcw = (sljit_u32)srcw; in sljit_emit_op1()
1736 sljit_u32 op_types,
1843 sljit_u32 op_types,
2680 void *instruction, sljit_u32 size)
2699 static sljit_u32 sse2_data[3 + (4 * 4)];
2700 static sljit_u32 *sse2_buffer;
[all …]
DsljitNativeS390X.c605 SLJIT_S390X_RILA(nihf, 0xc00a00000000, sljit_u32)
608 SLJIT_S390X_RILA(xilf, 0xc00700000000, sljit_u32)
611 SLJIT_S390X_RILA(iihf, 0xc00800000000, sljit_u32)
612 SLJIT_S390X_RILA(iilf, 0xc00900000000, sljit_u32)
618 SLJIT_S390X_RILA(llihf, 0xc00e00000000, sljit_u32)
619 SLJIT_S390X_RILA(llilf, 0xc00f00000000, sljit_u32)
622 SLJIT_S390X_RILA(slfi, 0xc20500000000, sljit_u32)
908 return push_inst(compiler, llilf(target, (sljit_u32)v)); in push_load_imm_inst()
911 return push_inst(compiler, llihf(target, (sljit_u32)((sljit_uw)v >> 32))); in push_load_imm_inst()
913 FAIL_IF(push_inst(compiler, llilf(target, (sljit_u32)v))); in push_load_imm_inst()
[all …]
DsljitNativePPC_32.c48 sljit_u32 imm; in emit_single_op()
304 imm = (sljit_u32)(-(sljit_s32)imm); in emit_single_op()
DsljitNativeRISCV_common.c38 typedef sljit_u32 sljit_ins;
287 static SLJIT_INLINE void load_addr_to_reg(void *dst, sljit_u32 reg) in load_addr_to_reg()
1721 …_U32, INT_DATA | MOVE_OP, dst, dstw, TMP_REG1, 0, src, (src & SLJIT_IMM) ? (sljit_u32)srcw : srcw); in sljit_emit_op1()
1963 void *instruction, sljit_u32 size) in sljit_emit_op_custom()
1983 # define flags (sljit_u32)0 in sljit_emit_fop1_conv_sw_from_f64()
1985 sljit_u32 flags = ((sljit_u32)(GET_OPCODE(op) == SLJIT_CONV_SW_FROM_F64)) << 21; in sljit_emit_fop1_conv_sw_from_f64()
2017 sljit_u32 flags = ((sljit_u32)(GET_OPCODE(op) == SLJIT_CONV_F64_FROM_SW)) << 21; in sljit_emit_fop1_conv_f64_from_sw()
2443 set_jump(jump, compiler, (sljit_u32)((type & SLJIT_REWRITABLE_JUMP) | IS_COND)); in sljit_emit_cmp()
DsljitLir.h481 sljit_u32 imm;
1695 void *instruction, sljit_u32 size);
DsljitNativeMIPS_common.c68 typedef sljit_u32 sljit_ins;
520 static SLJIT_INLINE void load_addr_to_reg(void *dst, sljit_u32 reg) in load_addr_to_reg()
2282 …_U32, INT_DATA | MOVE_OP, dst, dstw, TMP_REG1, 0, src, (src & SLJIT_IMM) ? (sljit_u32)srcw : srcw); in sljit_emit_op1()
2534 void *instruction, sljit_u32 size) in sljit_emit_op_custom()
2554 # define flags (sljit_u32)0 in sljit_emit_fop1_conv_sw_from_f64()
2556 sljit_u32 flags = ((sljit_u32)(GET_OPCODE(op) == SLJIT_CONV_SW_FROM_F64)) << 21; in sljit_emit_fop1_conv_sw_from_f64()
2587 # define flags (sljit_u32)0 in sljit_emit_fop1_conv_f64_from_sw()
2589 sljit_u32 flags = ((sljit_u32)(GET_OPCODE(op) == SLJIT_CONV_F64_FROM_SW)) << 21; in sljit_emit_fop1_conv_f64_from_sw()
2896 sljit_u32 flags = 0; in sljit_emit_jump()
DsljitNativePPC_64.c150 sljit_u32 imm; in emit_single_op()
479 imm = (sljit_u32)(-(sljit_s32)imm); in emit_single_op()
DsljitConfigInternal.h427 typedef unsigned int sljit_u32; typedef
DsljitNativePPC_common.c34 typedef sljit_u32 sljit_ins;
377 sljit_u32 reg = *inst; in put_label_set()
1394 return EMIT_MOV(SLJIT_MOV_U32, INT_DATA, (sljit_u32)); in sljit_emit_op1()
1870 void *instruction, sljit_u32 size) in sljit_emit_op_custom()
2303 set_jump(jump, compiler, (sljit_u32)type & SLJIT_REWRITABLE_JUMP); in sljit_emit_jump()
2426 sljit_u32 bit, from_xer; in sljit_emit_op_flags()
DsljitLir.c384 && sizeof(sljit_s32) == 4 && sizeof(sljit_u32) == 4 in sljit_create_compiler()
711 …JIT_INLINE void set_jump(struct sljit_jump *jump, struct sljit_compiler *compiler, sljit_u32 flags) in set_jump()
1538 void *instruction, sljit_u32 size) in check_sljit_emit_op_custom()
1541 sljit_u32 i; in check_sljit_emit_op_custom()
2879 void *instruction, sljit_u32 size) in sljit_emit_op_custom()
/third_party/pcre2/pcre2/src/
Dpcre2_jit_simd_inc.h53 static SLJIT_INLINE sljit_u32 max_fast_forward_char_pair_offset(void) in max_fast_forward_char_pair_offset()
87 sljit_u32 value = chr; in character_to_int32()
222 sljit_u32 bit = 0; in fast_forward_char_simd()
383 sljit_u32 bit = 0; in fast_requested_char_simd()
508 sljit_u32 bit1 = 0; in fast_forward_char_pair_simd()
509 sljit_u32 bit2 = 0; in fast_forward_char_pair_simd()
510 sljit_u32 diff = IN_UCHARS(offs1 - offs2); in fast_forward_char_pair_simd()
822 # define VLD1Q(X) vld1q_u32((sljit_u32 *)(X))
975 static SLJIT_INLINE sljit_u32 max_fast_forward_char_pair_offset(void) in max_fast_forward_char_pair_offset()
1052 sljit_u32 diff = IN_UCHARS(offs1 - offs2); in fast_forward_char_pair_simd()
[all …]
Dpcre2_jit_neon_inc.h117 const sljit_u32 diff = IN_UCHARS(offs1 - offs2); in FF_FUN()
136 sljit_u32 bit1 = char1a ^ char1b; in FF_FUN()
158 sljit_u32 bit2 = char2a ^ char2b; in FF_FUN()
Dpcre2_jit_compile.c190 sljit_u32 limit_match;
191 sljit_u32 oveccount;
192 sljit_u32 options;
201 sljit_u32 top_bracket;
202 sljit_u32 limit_match;
443 sljit_u32 nlmax;
444 sljit_u32 nlmin;
447 sljit_u32 bsr_nlmax;
448 sljit_u32 bsr_nlmin;
523 sljit_u32 asuchars[1];
[all …]