Searched refs:op (Results 1 - 25 of 1788) sorted by relevance

1234567891011>>

/xsrc/external/mit/MesaLib/dist/src/panfrost/midgard/
H A Dmidgard_ops.h35 #define OP_IS_ATOMIC(op) (load_store_opcode_props[op].props & LDST_ATOMIC)
36 #define OP_USES_ATTRIB(op) (load_store_opcode_props[op].props & LDST_ATTRIB)
37 #define OP_IS_STORE(op) (load_store_opcode_props[op].props & LDST_STORE)
38 #define OP_HAS_ADDRESS(op) (load_store_opcode_props[op].props & LDST_ADDRESS)
44 midgard_is_integer_op(int op) argument
46 return (op >
50 midgard_is_unsigned_op(int op) argument
84 midgard_is_integer_out_op(int op) argument
95 effective_writemask(midgard_alu_op op,unsigned existing_mask) argument
[all...]
H A Dhelpers.h30 #define OP_IS_LOAD_VARY_F(op) (\
31 op == midgard_op_ld_vary_16 || \
32 op == midgard_op_ld_vary_32 \
35 #define OP_IS_PROJECTION(op) ( \
36 op == midgard_op_ldst_perspective_div_y || \
37 op == midgard_op_ldst_perspective_div_z || \
38 op == midgard_op_ldst_perspective_div_w \
41 #define OP_IS_VEC4_ONLY(op) ( \
42 OP_IS_PROJECTION(op) || \
43 op
[all...]
/xsrc/external/mit/MesaLib/src/compiler/glsl/
H A Dir_expression_operation_constant.h3 for (unsigned c = 0; c < op[0]->type->components(); c++) {
4 switch (op[0]->type->base_type) {
6 data.u[c] = ~ op[0]->value.u[c];
9 data.i[c] = ~ op[0]->value.i[c];
12 data.u64[c] = ~ op[0]->value.u64[c];
15 data.i64[c] = ~ op[0]->value.i64[c];
24 for (unsigned c = 0; c < op[0]->type->components(); c++) {
25 switch (op[0]->type->base_type) {
27 data.b[c] = !op[0]->value.b[c];
36 for (unsigned c = 0; c < op[
[all...]
/xsrc/external/mit/xf86-video-geode/dist/src/
H A Dgeode_blend.h37 #define usesPasses(op) ((( \
41 0 ) >> (op)) & 1)
44 #define usesSrcAlpha(op) ((( \
51 0 ) >> (op)) & 1)
54 #define usesDstAlpha(op) ((( \
61 0 ) >> (op)) & 1)
64 #define usesChanB0(op) ((( \
72 0 ) >> (op)) & 1)
75 #define usesChanB1(op) ((( \
79 0 ) >> (op))
[all...]
/xsrc/external/mit/MesaLib.old/src/compiler/glsl/
H A Dir_expression_operation_constant.h3 for (unsigned c = 0; c < op[0]->type->components(); c++) {
4 switch (op[0]->type->base_type) {
6 data.u[c] = ~ op[0]->value.u[c];
9 data.i[c] = ~ op[0]->value.i[c];
12 data.u64[c] = ~ op[0]->value.u64[c];
15 data.i64[c] = ~ op[0]->value.i64[c];
24 for (unsigned c = 0; c < op[0]->type->components(); c++) {
25 switch (op[0]->type->base_type) {
27 data.b[c] = !op[0]->value.b[c];
36 for (unsigned c = 0; c < op[
[all...]
/xsrc/external/mit/xf86-video-intel-old/dist/src/
H A Di915_3d.h219 struct i915_fs_op op; local in function:_i915_fs_dcl
221 op.ui[0] = D0_DCL | (REG_TYPE(reg) << D0_TYPE_SHIFT) |
223 op.ui[1] = 0;
224 op.ui[2] = 0;
226 op.ui[0] |= D0_CHANNEL_ALL;
228 return op;
247 struct i915_fs_op op; local in function:_i915_fs_texld
249 op.ui[0] = 0;
250 op.ui[1] = 0;
251 op
275 struct i915_fs_op op; local in function:_i915_fs_arith
[all...]
/xsrc/external/mit/MesaLib.old/dist/src/compiler/nir/
H A Dnir_lower_bool_to_float.c48 const nir_op_info *op_info = &nir_op_infos[alu->op];
54 switch (alu->op) {
61 case nir_op_b2f32: alu->op = nir_op_fmov; break;
62 case nir_op_b2i32: alu->op = nir_op_fmov; break;
69 case nir_op_flt: alu->op = nir_op_slt; break;
70 case nir_op_fge: alu->op = nir_op_sge; break;
71 case nir_op_feq: alu->op = nir_op_seq; break;
72 case nir_op_fne: alu->op = nir_op_sne; break;
73 case nir_op_ilt: alu->op = nir_op_slt; break;
74 case nir_op_ige: alu->op
[all...]
H A Dnir_lower_bool_to_int32.c47 const nir_op_info *op_info = &nir_op_infos[alu->op];
51 switch (alu->op) {
63 case nir_op_f2b1: alu->op = nir_op_f2b32; break;
64 case nir_op_i2b1: alu->op = nir_op_i2b32; break;
66 case nir_op_flt: alu->op = nir_op_flt32; break;
67 case nir_op_fge: alu->op = nir_op_fge32; break;
68 case nir_op_feq: alu->op = nir_op_feq32; break;
69 case nir_op_fne: alu->op = nir_op_fne32; break;
70 case nir_op_ilt: alu->op = nir_op_ilt32; break;
71 case nir_op_ige: alu->op
[all...]
/xsrc/external/mit/MesaLib/dist/src/panfrost/bifrost/
H A Dbi_builder.h.py84 def to_suffix(op):
85 return "_to" if op["dests"] > 0 else ""
94 I->op = BI_OPCODE_${opcode.replace('.', '_').upper()};
127 signatures = [signature(ops[op], modifiers, no_dests=True) for op in variants]
176 def modifier_signature(op):
177 return sorted([m for m in op["modifiers"].keys() if not should_skip(m)])
179 def signature(op, modifiers, typeful = False, sized = False, no_dests = False):
184 ["bi_index dest{}".format(i) for i in range(0 if no_dests else op["dests"])] +
185 ["bi_index src{}".format(i) for i in range(src_count(op))]
[all...]
/xsrc/external/mit/MesaLib/dist/src/compiler/nir/
H A Dnir_lower_bool_to_int32.c47 const nir_op_info *op_info = &nir_op_infos[alu->op];
51 switch (alu->op) {
68 case nir_op_f2b1: alu->op = nir_op_f2b32; break;
69 case nir_op_i2b1: alu->op = nir_op_i2b32; break;
77 alu->op = nir_op_mov;
80 case nir_op_flt: alu->op = nir_op_flt32; break;
81 case nir_op_fge: alu->op = nir_op_fge32; break;
82 case nir_op_feq: alu->op = nir_op_feq32; break;
83 case nir_op_fneu: alu->op = nir_op_fneu32; break;
84 case nir_op_ilt: alu->op
[all...]
H A Dnir_lower_int_to_float.c39 const nir_op_info *info = &nir_op_infos[alu->op];
56 switch (alu->op) {
65 case nir_op_b2i32: alu->op = nir_op_b2f32; break;
66 case nir_op_i2f32: alu->op = nir_op_mov; break;
67 case nir_op_u2f32: alu->op = nir_op_mov; break;
68 case nir_op_f2i32: alu->op = nir_op_ftrunc; break;
69 case nir_op_f2u32: alu->op = nir_op_ffloor; break;
70 case nir_op_i2b1: alu->op = nir_op_f2b1; break;
72 case nir_op_ilt: alu->op = nir_op_flt; break;
73 case nir_op_ige: alu->op
[all...]
H A Dnir_constant_expressions.h33 void nir_eval_const_opcode(nir_op op, nir_const_value *dest,
/xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/swr/rasterizer/common/
H A Dsimdlib_512_avx512_knights.inl32 #define SIMD_WRAPPER_1_(op, intrin) \
33 static SIMDINLINE Float SIMDCALL op(Float a) { return intrin(a); }
35 #define SIMD_WRAPPER_1(op) SIMD_WRAPPER_1_(op, _mm512_##op)
37 #define SIMD_WRAPPER_2_(op, intrin) \
38 static SIMDINLINE Float SIMDCALL op(Float a, Float b) { return _mm512_##intrin(a, b); }
39 #define SIMD_WRAPPER_2(op) SIMD_WRAPPER_2_(op, op)
[all...]
H A Dsimdlib_128_avx512_core.inl36 #define SIMD_WRAPPER_1_(op, intrin, mask) \
37 static SIMDINLINE Float SIMDCALL op(Float a) \
41 #define SIMD_WRAPPER_1(op) SIMD_WRAPPER_1_(op, op, __mmask16(0xf))
43 #define SIMD_WRAPPER_1I_(op, intrin, mask) \
45 static SIMDINLINE Float SIMDCALL op(Float a) \
49 #define SIMD_WRAPPER_1I(op) SIMD_WRAPPER_1I_(op, op, __mmask1
[all...]
H A Dsimdlib_256_avx512_core.inl36 #define SIMD_DWRAPPER_1_(op, intrin, mask) \
37 static SIMDINLINE Double SIMDCALL op(Double a) \
41 #define SIMD_DWRAPPER_1(op) SIMD_DWRAPPER_1_(op, op, __mmask8(0xf))
43 #define SIMD_DWRAPPER_1I_(op, intrin, mask) \
45 static SIMDINLINE Double SIMDCALL op(Double a) \
49 #define SIMD_DWRAPPER_1I(op) SIMD_DWRAPPER_1I_(op, op, __mmask
[all...]
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/swr/rasterizer/common/
H A Dsimdlib_512_avx512_knights.inl32 #define SIMD_WRAPPER_1_(op, intrin) \
33 static SIMDINLINE Float SIMDCALL op(Float a) { return intrin(a); }
35 #define SIMD_WRAPPER_1(op) SIMD_WRAPPER_1_(op, _mm512_##op)
37 #define SIMD_WRAPPER_2_(op, intrin) \
38 static SIMDINLINE Float SIMDCALL op(Float a, Float b) { return _mm512_##intrin(a, b); }
39 #define SIMD_WRAPPER_2(op) SIMD_WRAPPER_2_(op, op)
[all...]
H A Dsimdlib_128_avx512_core.inl36 #define SIMD_WRAPPER_1_(op, intrin, mask) \
37 static SIMDINLINE Float SIMDCALL op(Float a) \
41 #define SIMD_WRAPPER_1(op) SIMD_WRAPPER_1_(op, op, __mmask16(0xf))
43 #define SIMD_WRAPPER_1I_(op, intrin, mask) \
45 static SIMDINLINE Float SIMDCALL op(Float a) \
49 #define SIMD_WRAPPER_1I(op) SIMD_WRAPPER_1I_(op, op, __mmask1
[all...]
H A Dsimdlib_256_avx512_core.inl36 #define SIMD_DWRAPPER_1_(op, intrin, mask) \
37 static SIMDINLINE Double SIMDCALL op(Double a) \
41 #define SIMD_DWRAPPER_1(op) SIMD_DWRAPPER_1_(op, op, __mmask8(0xf))
43 #define SIMD_DWRAPPER_1I_(op, intrin, mask) \
45 static SIMDINLINE Double SIMDCALL op(Double a) \
49 #define SIMD_DWRAPPER_1I(op) SIMD_DWRAPPER_1I_(op, op, __mmask
[all...]
/xsrc/external/mit/MesaLib/dist/src/compiler/glsl/
H A Dhir_field_selection.cpp36 ir_rvalue *op; local in function:_mesa_ast_field_selection_to_hir
38 op = expr->subexpressions[0]->hir(instructions, state);
47 if (op->type->is_error()) {
49 } else if (op->type->is_struct() || op->type->is_interface()) {
50 result = new(ctx) ir_dereference_record(op,
58 } else if (op->type->is_vector() ||
59 (state->has_420pack() && op->type->is_scalar())) {
60 ir_swizzle *swiz = ir_swizzle::create(op,
62 op
[all...]
H A Dast_expr.cpp27 ast_expression::operator_string(enum ast_operators op) argument
75 assert((unsigned int)op < sizeof(operators) / sizeof(operators[0]));
77 return operators[op];
H A Dopt_add_neg_to_sub.h43 ir_expression *const op = ir->operands[i]->as_expression(); local in function:add_neg_to_sub_visitor::visit_leave
45 if (op != NULL && op->operation == ir_unop_neg) {
52 ir->operands[1] = op->operands[0];
/xsrc/external/mit/MesaLib.old/dist/src/compiler/glsl/
H A Dhir_field_selection.cpp36 ir_rvalue *op; local in function:_mesa_ast_field_selection_to_hir
38 op = expr->subexpressions[0]->hir(instructions, state);
47 if (op->type->is_error()) {
49 } else if (op->type->is_struct() || op->type->is_interface()) {
50 result = new(ctx) ir_dereference_record(op,
58 } else if (op->type->is_vector() ||
59 (state->has_420pack() && op->type->is_scalar())) {
60 ir_swizzle *swiz = ir_swizzle::create(op,
62 op
[all...]
H A Dast_expr.cpp27 ast_expression::operator_string(enum ast_operators op) argument
75 assert((unsigned int)op < sizeof(operators) / sizeof(operators[0]));
77 return operators[op];
H A Dopt_add_neg_to_sub.h43 ir_expression *const op = ir->operands[i]->as_expression(); local in function:add_neg_to_sub_visitor::visit_leave
45 if (op != NULL && op->operation == ir_unop_neg) {
52 ir->operands[1] = op->operands[0];
/xsrc/external/mit/xedit/dist/lisp/mp/
H A Dmpr.c54 mpr_init(mpr *op) argument
56 op->num.digs = mp_malloc(sizeof(BNS));
57 op->num.sign = 0;
58 op->num.size = op->num.alloc = 1;
59 op->num.digs[0] = 0;
61 op->den.digs = mp_malloc(sizeof(BNS));
62 op->den.sign = 0;
63 op->den.size = op
68 mpr_clear(mpr * op) argument
80 mpr_set(mpr * rop,mpr * op) argument
139 mpr_canonicalize(mpr * op) argument
272 mpr_inv(mpr * rop,mpr * op) argument
283 mpr_neg(mpr * rop,mpr * op) argument
290 mpr_abs(mpr * rop,mpr * op) argument
407 mpr_fiti(mpr * op) argument
413 mpr_getd(mpr * op) argument
419 mpr_getstr(char * str,mpr * op,int base) argument
[all...]

Completed in 30 milliseconds

1234567891011>>