Home
last modified time | relevance | path

Searched refs:dst_reg (Results 1 – 25 of 27) sorted by relevance

12

/external/mesa3d/src/mesa/drivers/dri/i965/
Dbrw_vec4.h42 class dst_reg; variable
108 explicit src_reg(dst_reg reg);
117 class dst_reg : public reg
134 dst_reg();
135 dst_reg(register_file file, int reg);
136 dst_reg(register_file file, int reg, const glsl_type *type, int writemask);
137 dst_reg(struct brw_reg reg);
138 dst_reg(class vec4_visitor *v, const struct glsl_type *type);
140 explicit dst_reg(src_reg reg);
162 dst_reg dst = dst_reg(),
[all …]
Dbrw_vec4_visitor.cpp34 enum opcode opcode, dst_reg dst, in vec4_instruction()
66 vec4_visitor::emit(enum opcode opcode, dst_reg dst, in emit()
75 vec4_visitor::emit(enum opcode opcode, dst_reg dst, src_reg src0, src_reg src1) in emit()
81 vec4_visitor::emit(enum opcode opcode, dst_reg dst, src_reg src0) in emit()
89 return emit(new(mem_ctx) vec4_instruction(this, opcode, dst_reg())); in emit()
94 vec4_visitor::op(dst_reg dst, src_reg src0) \
102 vec4_visitor::op(dst_reg dst, src_reg src0, src_reg src1) \
159 vec4_visitor::CMP(dst_reg dst, src_reg src0, src_reg src1, uint32_t condition) in CMP()
183 vec4_visitor::SCRATCH_READ(dst_reg dst, src_reg index) in SCRATCH_READ()
196 vec4_visitor::SCRATCH_WRITE(dst_reg dst, src_reg src, src_reg index) in SCRATCH_WRITE()
[all …]
Dbrw_vec4.cpp107 src_reg::src_reg(dst_reg reg) in src_reg()
148 dst_reg::init() in init()
155 dst_reg::dst_reg() in dst_reg() function in brw::dst_reg
160 dst_reg::dst_reg(register_file file, int reg) in dst_reg() function in brw::dst_reg
168 dst_reg::dst_reg(register_file file, int reg, const glsl_type *type, in dst_reg() function in brw::dst_reg
179 dst_reg::dst_reg(struct brw_reg reg) in dst_reg() function in brw::dst_reg
187 dst_reg::dst_reg(src_reg reg) in dst_reg() function in brw::dst_reg
675 dst_reg temp = dst_reg(this, glsl_type::vec4_type); in move_push_constants_to_pull_constants()
Dbrw_vec4_reg_allocate.cpp334 dst_reg temp = dst_reg(inst->src[i]); in spill_reg()
349 dst_reg spill_reg = inst->dst; in spill_reg()
Dbrw_fs_visitor.cpp1452 fs_reg dst_reg = reg; in visit() local
1461 dst_reg.type = src_reg.type; in visit()
1463 emit(BRW_OPCODE_MOV, dst_reg, src_reg); in visit()
1465 dst_reg.reg_offset++; in visit()
1476 dst_reg.type = src_reg.type; in visit()
1478 emit(BRW_OPCODE_MOV, dst_reg, src_reg); in visit()
1480 dst_reg.reg_offset++; in visit()
1489 emit(BRW_OPCODE_MOV, dst_reg, fs_reg(ir->value.f[i])); in visit()
1492 emit(BRW_OPCODE_MOV, dst_reg, fs_reg(ir->value.u[i])); in visit()
1495 emit(BRW_OPCODE_MOV, dst_reg, fs_reg(ir->value.i[i])); in visit()
[all …]
Dbrw_wm_fp.c134 static struct prog_dst_register dst_reg(GLuint file, GLuint idx) in dst_reg() function
155 return dst_reg(PROGRAM_UNDEFINED, 0); in dst_undef()
170 return dst_reg(PROGRAM_TEMPORARY, FIRST_INTERNAL_TEMP+(bit-1)); in get_temp()
370 struct prog_dst_register dst = dst_reg(PROGRAM_INPUT, idx); in emit_interp()
/external/mesa3d/src/mesa/program/
Dir_to_mesa.cpp62 class dst_reg;
93 explicit src_reg(dst_reg reg);
103 class dst_reg { class
105 dst_reg(gl_register_file file, int writemask) in dst_reg() function in dst_reg
114 dst_reg() in dst_reg() function in dst_reg
123 explicit dst_reg(src_reg reg);
133 src_reg::src_reg(dst_reg reg) in src_reg()
142 dst_reg::dst_reg(src_reg reg) in dst_reg() function in dst_reg
166 dst_reg dst;
286 dst_reg dst, src_reg src0);
[all …]
Dprogram_parse.y132 struct prog_dst_register dst_reg;
203 %type <dst_reg> dstReg maskedDstReg maskedAddrReg
215 %type <dst_reg> ccMaskRule ccTest ccMaskRule2 ccTest2 optionalCcMask
/external/mesa3d/src/gallium/drivers/i915/
Di915_state_emit.c425 int dst_reg, in emit_instruction() argument
433 A0_DEST(dst_reg) | in emit_instruction()
444 int dst_reg = in emit_srgb_fixup() local
456 emit_instruction(i915, A0_MAD, A0_DEST_CHANNEL_ALL, t1_reg, dst_reg, cst0_reg, cst1_reg); in emit_srgb_fixup()
461 emit_instruction(i915, A0_EXP, dst_mask & A0_DEST_CHANNEL_X, dst_reg, t1x_reg, 0, 0); in emit_srgb_fixup()
462 emit_instruction(i915, A0_EXP, dst_mask & A0_DEST_CHANNEL_Y, dst_reg, t1y_reg, 0, 0); in emit_srgb_fixup()
463 emit_instruction(i915, A0_EXP, dst_mask & A0_DEST_CHANNEL_Z, dst_reg, t1z_reg, 0, 0); in emit_srgb_fixup()
/external/valgrind/none/tests/s390x/
Dpfpo.c32 register dst_type dst_reg asm("f0"); \
38 :"=f"(dst_reg), "=d"(ret), "=d" (cc) \
41 dst_reg; \
/external/libvpx/libvpx/vpx_dsp/x86/
Dvariance_impl_avx2.c258 dst_reg = _mm256_loadu_si256((__m256i const *) (dst));
273 exp_dst_lo = _mm256_unpacklo_epi8(dst_reg, zero_reg); \
274 exp_dst_hi = _mm256_unpackhi_epi8(dst_reg, zero_reg); \
317 __m256i src_reg, dst_reg, exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi; in vpx_sub_pixel_variance32xh_avx2() local
511 __m256i src_reg, dst_reg, exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi; in vpx_sub_pixel_avg_variance32xh_avx2() local
/external/kernel-headers/original/uapi/linux/
Dbpf.h60 __u8 dst_reg:4; /* dest register */ member
/external/iproute2/include/linux/
Dbpf.h60 __u8 dst_reg:4; /* dest register */ member
/external/v8/src/arm/
Dmacro-assembler-arm.h746 int dst_reg = (instr & dst_mask) >> dst_reg_offset; in GetCodeMarker() local
753 (dst_reg == src_reg) && in GetCodeMarker()
754 (FIRST_IC_MARKER <= dst_reg) && (dst_reg < LAST_CODE_MARKER) in GetCodeMarker()
Dmacro-assembler-arm.cc1458 Register dst_reg = scratch0; in PrepareForTailCall() local
1459 add(dst_reg, fp, Operand(caller_args_count_reg, LSL, kPointerSizeLog2)); in PrepareForTailCall()
1460 add(dst_reg, dst_reg, in PrepareForTailCall()
1474 cmp(src_reg, dst_reg); in PrepareForTailCall()
1493 str(tmp_reg, MemOperand(dst_reg, -kPointerSize, PreIndex)); in PrepareForTailCall()
1499 mov(sp, dst_reg); in PrepareForTailCall()
/external/mesa3d/src/mesa/state_tracker/
Dst_glsl_to_tgsi.cpp4103 const st_dst_reg *dst_reg, in translate_dst() argument
4107 dst_reg->file, in translate_dst()
4108 dst_reg->index); in translate_dst()
4110 dst = ureg_writemask(dst, dst_reg->writemask); in translate_dst()
4114 else if (clamp_color && dst_reg->file == PROGRAM_OUTPUT) { in translate_dst()
4120 if (dst_reg->index == VERT_RESULT_COL0 || in translate_dst()
4121 dst_reg->index == VERT_RESULT_COL1 || in translate_dst()
4122 dst_reg->index == VERT_RESULT_BFC0 || in translate_dst()
4123 dst_reg->index == VERT_RESULT_BFC1) { in translate_dst()
4129 if (dst_reg->index >= FRAG_RESULT_COLOR) { in translate_dst()
[all …]
/external/pcre/dist/sljit/
DsljitNativeX86_common.c2960 sljit_si dst_reg, argument
2970 CHECK_ARGUMENT(FUNCTION_CHECK_IS_REG(dst_reg & ~SLJIT_INT_OP));
2976 !(dst_reg & SLJIT_INT_OP) ? "" : ".i",
2978 sljit_verbose_reg(compiler, dst_reg & ~SLJIT_INT_OP);
2989 compiler->mode32 = dst_reg & SLJIT_INT_OP;
2991 dst_reg &= ~SLJIT_INT_OP;
2999 inst = emit_x86_instruction(compiler, 2, dst_reg, 0, src, srcw);
DsljitLir.h1244 sljit_si dst_reg,
/external/v8/src/ppc/
Dmacro-assembler-ppc.h681 int dst_reg = (instr & dst_mask) >> dst_reg_offset; in GetCodeMarker() local
688 (dst_reg == src_reg) && (FIRST_IC_MARKER <= dst_reg) && in GetCodeMarker()
689 (dst_reg < LAST_CODE_MARKER) in GetCodeMarker()
Dmacro-assembler-ppc.cc1259 Register dst_reg = scratch0; in PrepareForTailCall() local
1260 ShiftLeftImm(dst_reg, caller_args_count_reg, Operand(kPointerSizeLog2)); in PrepareForTailCall()
1261 add(dst_reg, fp, dst_reg); in PrepareForTailCall()
1262 addi(dst_reg, dst_reg, in PrepareForTailCall()
1276 cmpl(src_reg, dst_reg); in PrepareForTailCall()
1299 StorePU(tmp_reg, MemOperand(dst_reg, -kPointerSize)); in PrepareForTailCall()
1303 mr(sp, dst_reg); in PrepareForTailCall()
/external/v8/src/s390/
Dmacro-assembler-s390.cc1181 Register dst_reg = scratch0; in PrepareForTailCall() local
1182 ShiftLeftP(dst_reg, caller_args_count_reg, Operand(kPointerSizeLog2)); in PrepareForTailCall()
1183 AddP(dst_reg, fp, dst_reg); in PrepareForTailCall()
1184 AddP(dst_reg, dst_reg, in PrepareForTailCall()
1199 CmpLogicalP(src_reg, dst_reg); in PrepareForTailCall()
1222 StoreP(tmp_reg, MemOperand(dst_reg, -kPointerSize)); in PrepareForTailCall()
1224 lay(dst_reg, MemOperand(dst_reg, -kPointerSize)); in PrepareForTailCall()
1228 LoadRR(sp, dst_reg); in PrepareForTailCall()
Dmacro-assembler-s390.h936 int dst_reg = (instr & dst_mask) >> dst_reg_offset; in GetCodeMarker() local
943 (dst_reg == src_reg) && (FIRST_IC_MARKER <= dst_reg) && in GetCodeMarker()
944 (dst_reg < LAST_CODE_MARKER) in GetCodeMarker()
/external/v8/src/arm64/
Dmacro-assembler-arm64.cc2372 Register dst_reg = scratch0; in PrepareForTailCall() local
2373 __ add(dst_reg, fp, Operand(caller_args_count_reg, LSL, kPointerSizeLog2)); in PrepareForTailCall()
2374 __ add(dst_reg, dst_reg, in PrepareForTailCall()
2388 __ Cmp(src_reg, dst_reg); in PrepareForTailCall()
2407 __ Str(tmp_reg, MemOperand(dst_reg, -kPointerSize, PreIndex)); in PrepareForTailCall()
2413 __ Mov(jssp, dst_reg); in PrepareForTailCall()
/external/v8/src/mips/
Dmacro-assembler-mips.cc5016 Register dst_reg = scratch0; in PrepareForTailCall() local
5017 Lsa(dst_reg, fp, caller_args_count_reg, kPointerSizeLog2); in PrepareForTailCall()
5018 Addu(dst_reg, dst_reg, in PrepareForTailCall()
5032 Check(lo, kStackAccessBelowStackPointer, src_reg, Operand(dst_reg)); in PrepareForTailCall()
5050 Subu(dst_reg, dst_reg, Operand(kPointerSize)); in PrepareForTailCall()
5052 sw(tmp_reg, MemOperand(dst_reg)); in PrepareForTailCall()
5057 mov(sp, dst_reg); in PrepareForTailCall()
/external/v8/src/mips64/
Dmacro-assembler-mips64.cc5149 Register dst_reg = scratch0; in PrepareForTailCall() local
5150 Dlsa(dst_reg, fp, caller_args_count_reg, kPointerSizeLog2); in PrepareForTailCall()
5151 Daddu(dst_reg, dst_reg, in PrepareForTailCall()
5165 Check(lo, kStackAccessBelowStackPointer, src_reg, Operand(dst_reg)); in PrepareForTailCall()
5183 Dsubu(dst_reg, dst_reg, Operand(kPointerSize)); in PrepareForTailCall()
5185 sd(tmp_reg, MemOperand(dst_reg)); in PrepareForTailCall()
5190 mov(sp, dst_reg); in PrepareForTailCall()

12