Home
last modified time | relevance | path

Searched refs:sljit_u8 (Results 1 – 21 of 21) sorted by relevance

/external/pcre/dist2/src/sljit/
DsljitNativeX86_64.c31 sljit_u8 *inst; in emit_load_imm64()
33 inst = (sljit_u8*)ensure_buf(compiler, 1 + 2 + sizeof(sljit_sw)); in emit_load_imm64()
42 static sljit_u8* generate_far_jump_code(struct sljit_jump *jump, sljit_u8 *code_ptr) in generate_far_jump_code()
77 static sljit_u8* generate_put_label_code(struct sljit_put_label *put_label, sljit_u8 *code_ptr, slj… in generate_put_label_code()
87 code_ptr = (sljit_u8*)put_label->addr - 2 - sizeof(sljit_uw); in generate_put_label_code()
93 code_ptr[0] = (sljit_u8)(code_ptr[0] & ~0x08); in generate_put_label_code()
117 code_ptr[0] = (sljit_u8)(code_ptr[0] & ~0x4); in generate_put_label_code()
119 code_ptr[2] = (sljit_u8)(code_ptr[2] & ~(0x7 << 3)); in generate_put_label_code()
121 code_ptr = (sljit_u8*)(put_label->addr - (2 + sizeof(sljit_uw)) + sizeof(sljit_s32)); in generate_put_label_code()
132 sljit_u8 *inst; in sljit_emit_enter()
[all …]
DsljitNativeX86_common.c73 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 3] = {
98 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 4] = {
102 static const sljit_u8 reg_lmap[SLJIT_NUMBER_OF_REGISTERS + 4] = {
107 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 4] = {
111 static const sljit_u8 reg_lmap[SLJIT_NUMBER_OF_REGISTERS + 4] = {
117 static const sljit_u8 freg_map[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 1] = {
121 static const sljit_u8 freg_lmap[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 1] = {
374 static sljit_u8 get_jump_code(sljit_s32 type) in get_jump_code()
431 static sljit_u8* generate_far_jump_code(struct sljit_jump *jump, sljit_u8 *code_ptr, sljit_sw execu…
433 static sljit_u8* generate_far_jump_code(struct sljit_jump *jump, sljit_u8 *code_ptr);
[all …]
DsljitNativeX86_32.c29 static sljit_s32 emit_do_imm(struct sljit_compiler *compiler, sljit_u8 opcode, sljit_sw imm) in emit_do_imm()
31 sljit_u8 *inst; in emit_do_imm()
33 inst = (sljit_u8*)ensure_buf(compiler, 1 + 1 + sizeof(sljit_sw)); in emit_do_imm()
41 static sljit_u8* generate_far_jump_code(struct sljit_jump *jump, sljit_u8 *code_ptr, sljit_sw execu… in generate_far_jump_code()
73 sljit_u8 *inst; in sljit_emit_enter()
111 inst = (sljit_u8*)ensure_buf(compiler, 1 + size); in sljit_emit_enter()
203 inst = (sljit_u8*)ensure_buf(compiler, 1 + 2); in sljit_emit_enter()
231 inst = (sljit_u8*)ensure_buf(compiler, 1 + 6); in sljit_emit_enter()
292 sljit_u8 *inst; in sljit_emit_return()
319 inst = (sljit_u8*)ensure_buf(compiler, 1 + size); in sljit_emit_return()
[all …]
DsljitUtils.c188 stack->min_start = (sljit_u8 *)ptr; in sljit_allocate_stack()
202 SLJIT_API_FUNC_ATTRIBUTE sljit_u8 *SLJIT_FUNC sljit_stack_resize(struct sljit_stack *stack, sljit_u… in sljit_stack_resize()
258 stack->min_start = (sljit_u8 *)ptr; in sljit_allocate_stack()
280 stack->min_start = (sljit_u8 *)ptr; in sljit_allocate_stack()
289 SLJIT_API_FUNC_ATTRIBUTE sljit_u8 *SLJIT_FUNC sljit_stack_resize(struct sljit_stack *stack, sljit_u… in sljit_stack_resize()
DsljitLir.h348 sljit_u8 memory[1];
432 sljit_u8 *cpool_unique;
1447 sljit_u8 *top;
1450 sljit_u8 *end;
1452 sljit_u8 *start;
1454 sljit_u8 *min_start;
1467 SLJIT_API_FUNC_ATTRIBUTE sljit_u8 *SLJIT_FUNC sljit_stack_resize(struct sljit_stack *stack, sljit_u…
DsljitProtExecAllocator.c280 ((struct block_header*)(((sljit_u8*)base) + offset))
282 ((struct free_block*)(((sljit_u8*)base) + offset))
364 executable_offset = (sljit_sw)((sljit_u8*)chunk_header->executable - (sljit_u8*)chunk_header); in sljit_malloc_exec()
DsljitExecAllocator.c213 ((struct block_header*)(((sljit_u8*)base) + offset))
215 ((struct free_block*)(((sljit_u8*)base) + offset))
216 #define MEM_START(base) ((void*)(((sljit_u8*)base) + sizeof(struct block_header)))
DsljitNativeS390X.c47 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 4] = {
176 static SLJIT_INLINE sljit_u8 get_cc(sljit_s32 type) { in get_cc()
177 const sljit_u8 eq = 1 << 3; /* equal {,to zero} */ in get_cc()
178 const sljit_u8 lt = 1 << 2; /* less than {,zero} */ in get_cc()
179 const sljit_u8 gt = 1 << 1; /* greater than {,zero} */ in get_cc()
180 const sljit_u8 ov = 1 << 0; /* {overflow,NaN} */ in get_cc()
223 return (sljit_u8)-1; in get_cc()
799 SLJIT_S390X_INSTRUCTION(name, sljit_gpr dst, sljit_gpr src, sljit_u8 start, sljit_u8 end, sljit_u8 …
944 …S390X_INSTRUCTION(risbhgz, sljit_gpr dst, sljit_gpr src, sljit_u8 start, sljit_u8 end, sljit_u8 ro… in SLJIT_S390X_INSTRUCTION()
1345 SLJIT_ASSERT((sljit_u8 *)code + ins_size == code_ptr); in sljit_generate_code()
[all …]
DsljitNativeMIPS_32.c454 sljit_u8 offsets[4]; in call_with_args()
465 offsets[arg_count] = (sljit_u8)stack_offset; in call_with_args()
477 offsets[arg_count] = (sljit_u8)stack_offset; in call_with_args()
487 offsets[arg_count] = (sljit_u8)stack_offset; in call_with_args()
DsljitLir.c277 #define SLJIT_ADD_EXEC_OFFSET(ptr, exec_offset) ((sljit_u8 *)(ptr) + (exec_offset))
279 #define SLJIT_ADD_EXEC_OFFSET(ptr, exec_offset) ((sljit_u8 *)(ptr))
374 sizeof(sljit_s8) == 1 && sizeof(sljit_u8) == 1 in sljit_create_compiler()
423 + CPOOL_SIZE * sizeof(sljit_u8), allocator_data); in sljit_create_compiler()
430 compiler->cpool_unique = (sljit_u8*)(compiler->cpool + CPOOL_SIZE); in sljit_create_compiler()
553 sljit_u8 *ret; in ensure_buf()
572 sljit_u8 *ret; in ensure_abuf()
1400 fprintf(compiler->verbose, " 0x%x", ((sljit_u8*)instruction)[i]); in check_sljit_emit_op_custom()
DsljitNativeARM_32.c63 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 5] = {
67 static const sljit_u8 freg_map[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 3] = {
197 sljit_u8* cpool_unique_ptr; in push_inst_with_literal()
1783 …ALLOW_ANY_IMM | BYTE_SIZE, dst, dstw, TMP_REG1, 0, src, (src & SLJIT_IMM) ? (sljit_u8)srcw : srcw); in sljit_emit_op1()
2279 sljit_u8 offsets[4]; in softfloat_call_with_args()
2291 offsets[arg_count] = (sljit_u8)stack_offset; in softfloat_call_with_args()
2299 offsets[arg_count] = (sljit_u8)stack_offset; in softfloat_call_with_args()
2305 offsets[arg_count] = (sljit_u8)stack_offset; in softfloat_call_with_args()
DsljitNativeARM_T2_32.c48 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 5] = {
52 static const sljit_u8 freg_map[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 3] = {
1368 srcw = (sljit_u8)srcw; in sljit_emit_op1()
1876 sljit_u8 offsets[4]; in softfloat_call_with_args()
1888 offsets[arg_count] = (sljit_u8)stack_offset; in softfloat_call_with_args()
1896 offsets[arg_count] = (sljit_u8)stack_offset; in softfloat_call_with_args()
1902 offsets[arg_count] = (sljit_u8)stack_offset; in softfloat_call_with_args()
DsljitConfigInternal.h391 typedef unsigned char sljit_u8; typedef
DsljitNativeSPARC_common.c100 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 6] = {
104 static const sljit_u8 freg_map[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 3] = {
911 …MOV_U8, flags | BYTE_DATA, dst, dstw, TMP_REG1, 0, src, (src & SLJIT_IMM) ? (sljit_u8)srcw : srcw); in sljit_emit_op1()
DsljitNativeMIPS_common.c82 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 5] = {
88 static const sljit_u8 freg_map[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 4] = {
94 static const sljit_u8 freg_map[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 4] = {
1365 …, SLJIT_MOV_U8, BYTE_DATA, dst, dstw, TMP_REG1, 0, src, (src & SLJIT_IMM) ? (sljit_u8)srcw : srcw); in sljit_emit_op1()
DsljitNativeARM_64.c46 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 8] = {
50 static const sljit_u8 freg_map[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 3] = {
1185 srcw = (sljit_u8)srcw; in sljit_emit_op1()
DsljitNativePPC_common.c107 static const sljit_u8 reg_map[SLJIT_NUMBER_OF_REGISTERS + 7] = {
111 static const sljit_u8 freg_map[SLJIT_NUMBER_OF_FLOAT_REGISTERS + 3] = {
1264 return EMIT_MOV(SLJIT_MOV_U8, BYTE_DATA, (sljit_u8)); in sljit_emit_op1()
/external/pcre/dist2/src/
Dpcre2_jit_neon_inc.h85 static sljit_u8* SLJIT_FUNC FF_FUN(sljit_u8 *str_end, sljit_u8 *str_ptr, sljit_uw offs1, sljit_uw o… in FF_FUN()
97 sljit_u8 c1 = ic.c.c1; in FF_FUN()
101 sljit_u8 c1 = ic.c.c1; in FF_FUN()
103 sljit_u8 c2 = ic.c.c2; in FF_FUN()
107 sljit_u8 c1 = ic.c.c1; in FF_FUN()
109 sljit_u8 mask = ic.c.c2; in FF_FUN()
186 sljit_u8 *p1 = str_ptr - diff; in FF_FUN()
189 str_ptr = (sljit_u8 *) ((uint64_t)str_ptr & ~0xf); in FF_FUN()
Dpcre2_jit_simd_inc.h78 sljit_u8 instruction[5]; in load_from_mem_sse2()
84 instruction[0] = ((sljit_u8)offset & 0xf) == 0 ? 0x66 : 0xf3; in load_from_mem_sse2()
96 instruction[4] = (sljit_u8)offset; in load_from_mem_sse2()
109 sljit_u8 instruction[4]; in fast_forward_char_pair_sse2_compare()
195 sljit_u8 instruction[8]; in fast_forward_char_simd()
356 sljit_u8 instruction[8]; in fast_requested_char_simd()
519 sljit_u8 instruction[8]; in fast_forward_char_pair_simd()
775 static SLJIT_INLINE int utf_continue(sljit_u8 *s) in utf_continue()
790 # define VLD1Q(X) vld1q_u8((sljit_u8 *)(X))
985 static SLJIT_INLINE vect_t shift_left_n_lanes(vect_t a, sljit_u8 n) in shift_left_n_lanes()
Dpcre2_jit_match.c49 sljit_u8 local_space[MACHINE_STACK_SIZE]; in jit_machine_stack_exec()
Dpcre2_jit_compile.c361 sljit_u8 count;
363 sljit_u8 last_count;
383 sljit_u8 *optimized_cbracket;
385 sljit_u8 *then_offsets;
418 const sljit_u8 *fcc;
515 sljit_u8 asbyte;
516 sljit_u8 asuchars[4];
527 sljit_u8 asbyte;
528 sljit_u8 asuchars[4];
2964 static SLJIT_INLINE PCRE2_SPTR set_then_offsets(compiler_common *common, PCRE2_SPTR cc, sljit_u8 *c… in set_then_offsets()
[all …]