Home
last modified time | relevance | path

Searched refs:prim_type (Results 1 – 25 of 37) sorted by relevance

12

/external/tensorflow/tensorflow/compiler/xla/service/gpu/
Delemental_ir_emitter.cc202 StatusOr<llvm::Value*> GpuElementalIrEmitter::EmitLog(PrimitiveType prim_type, in EmitLog() argument
204 return EmitDeviceMathCall(TargetDeviceFunctionID::kLog, {value}, {prim_type}, in EmitLog()
205 prim_type); in EmitLog()
208 StatusOr<llvm::Value*> GpuElementalIrEmitter::EmitLog1p(PrimitiveType prim_type, in EmitLog1p() argument
211 {prim_type}, prim_type); in EmitLog1p()
214 StatusOr<llvm::Value*> GpuElementalIrEmitter::EmitSin(PrimitiveType prim_type, in EmitSin() argument
216 return EmitDeviceMathCall(TargetDeviceFunctionID::kSin, {value}, {prim_type}, in EmitSin()
217 prim_type); in EmitSin()
220 StatusOr<llvm::Value*> GpuElementalIrEmitter::EmitCos(PrimitiveType prim_type, in EmitCos() argument
222 return EmitDeviceMathCall(TargetDeviceFunctionID::kCos, {value}, {prim_type}, in EmitCos()
[all …]
Delemental_ir_emitter.h55 StatusOr<llvm::Value*> EmitLog(PrimitiveType prim_type,
58 StatusOr<llvm::Value*> EmitLog1p(PrimitiveType prim_type,
61 StatusOr<llvm::Value*> EmitSin(PrimitiveType prim_type,
64 StatusOr<llvm::Value*> EmitCos(PrimitiveType prim_type,
67 StatusOr<llvm::Value*> EmitExp(PrimitiveType prim_type, llvm::Value* value,
70 StatusOr<llvm::Value*> EmitExpm1(PrimitiveType prim_type,
73 StatusOr<llvm::Value*> EmitSqrt(PrimitiveType prim_type,
76 StatusOr<llvm::Value*> EmitRsqrt(PrimitiveType prim_type,
79 StatusOr<llvm::Value*> EmitPow(PrimitiveType prim_type, llvm::Value* lhs,
83 StatusOr<llvm::Value*> EmitAtan2(PrimitiveType prim_type, llvm::Value* lhs,
[all …]
/external/tensorflow/tensorflow/compiler/xla/service/
Delemental_ir_emitter.h121 virtual StatusOr<llvm::Value*> EmitAtan2(PrimitiveType prim_type,
125 virtual StatusOr<llvm::Value*> EmitLog(PrimitiveType prim_type,
128 virtual StatusOr<llvm::Value*> EmitSqrt(PrimitiveType prim_type,
131 virtual StatusOr<llvm::Value*> EmitCbrt(PrimitiveType prim_type,
134 virtual StatusOr<llvm::Value*> EmitRsqrt(PrimitiveType prim_type,
137 virtual StatusOr<llvm::Value*> EmitLog1p(PrimitiveType prim_type,
140 virtual StatusOr<llvm::Value*> EmitSin(PrimitiveType prim_type,
143 virtual StatusOr<llvm::Value*> EmitCos(PrimitiveType prim_type,
146 virtual StatusOr<llvm::Value*> EmitExp(PrimitiveType prim_type,
150 virtual StatusOr<llvm::Value*> EmitExpm1(PrimitiveType prim_type,
[all …]
Delemental_ir_emitter.cc901 ElementalIrEmitter::EmitComplexAbsHelper(PrimitiveType prim_type, in EmitComplexAbsHelper() argument
917 TF_ASSIGN_OR_RETURN(llvm::Value * sqrt, EmitSqrt(prim_type, one_p_div_sq)); in EmitComplexAbsHelper()
922 PrimitiveType prim_type, llvm::Value* operand_value) { in EmitComplexAbs() argument
928 EmitComplexAbsHelper(prim_type, operand_value, /*return_sqrt=*/true)); in EmitComplexAbs()
938 PrimitiveType prim_type, llvm::Value* operand_value) { in EmitSqrtComplexAbs() argument
944 EmitComplexAbsHelper(prim_type, operand_value, /*return_sqrt=*/false)); in EmitSqrtComplexAbs()
945 TF_ASSIGN_OR_RETURN(llvm::Value * sqrt_max, EmitSqrt(prim_type, max)); in EmitSqrtComplexAbs()
947 EmitPow(prim_type, one_p_div_sq, in EmitSqrtComplexAbs()
958 PrimitiveType prim_type, llvm::Value* operand_value) { in EmitRsqrtComplexAbs() argument
964 EmitComplexAbsHelper(prim_type, operand_value, /*return_sqrt=*/true)); in EmitRsqrtComplexAbs()
[all …]
/external/mesa3d/src/gallium/auxiliary/util/
Du_prim.h287 u_base_prim_type(enum pipe_prim_type prim_type) in u_base_prim_type() argument
289 switch(prim_type) { in u_base_prim_type()
308 return prim_type; in u_base_prim_type()
313 u_vertices_for_prims(enum pipe_prim_type prim_type, int count) in u_vertices_for_prims() argument
321 assert(prim_type == u_base_prim_type(prim_type) && in u_vertices_for_prims()
322 prim_type != PIPE_PRIM_PATCHES && prim_type != PIPE_PRIM_POLYGON); in u_vertices_for_prims()
324 const struct u_prim_vertex_count *info = u_prim_vertex_count(prim_type); in u_vertices_for_prims()
Du_draw_quad.c47 uint prim_type, in util_draw_vertex_buffer() argument
65 cso_draw_arrays(cso, prim_type, 0, num_verts); in util_draw_vertex_buffer()
68 util_draw_arrays(pipe, prim_type, 0, num_verts); in util_draw_vertex_buffer()
79 uint prim_type, uint num_verts, uint num_attribs) in util_draw_user_vertex_buffer() argument
92 cso_draw_arrays(cso, prim_type, 0, num_verts); in util_draw_user_vertex_buffer()
Du_draw_quad.h47 uint offset, uint prim_type, uint num_attribs,
52 uint prim_type, uint num_verts, uint num_attribs);
/external/tensorflow/tensorflow/compiler/xla/service/cpu/
Delemental_ir_emitter.cc37 PrimitiveType prim_type, llvm::Value* lhs, llvm::Value* rhs, in EmitAtan2() argument
41 switch (prim_type) { in EmitAtan2()
73 StatusOr<llvm::Value*> CpuElementalIrEmitter::EmitTanh(PrimitiveType prim_type, in EmitTanh() argument
77 switch (prim_type) { in EmitTanh()
Delemental_ir_emitter.h39 StatusOr<llvm::Value*> EmitAtan2(PrimitiveType prim_type, llvm::Value* lhs,
42 StatusOr<llvm::Value*> EmitTanh(PrimitiveType prim_type,
/external/mesa3d/src/gallium/tests/unit/
Du_prim_verts_test.c7 enum pipe_prim_type prim_type; member
35 uint32_t n = u_vertices_for_prims(info->prim_type, info->count); in main()
38 info->expected, info->count, u_prim_name(info->prim_type), n); in main()
/external/mesa3d/src/compiler/glsl/
Dast_type.cpp133 if (qualifier.flags.q.prim_type && new_qualifier.flags.q.prim_type in validate_prim_type()
134 && qualifier.prim_type != new_qualifier.prim_type) { in validate_prim_type()
315 if (q.flags.q.prim_type) { in merge_qualifier()
317 this->flags.q.prim_type = 1; in merge_qualifier()
318 this->prim_type = q.prim_type; in merge_qualifier()
512 if (this->flags.q.prim_type) { in validate_out_qualifier()
514 switch (this->prim_type) { in validate_out_qualifier()
534 valid_out_mask.flags.q.prim_type = 1; in validate_out_qualifier()
606 if (this->flags.q.prim_type) { in validate_in_qualifier()
608 switch (this->prim_type) { in validate_in_qualifier()
[all …]
Dast.h566 unsigned prim_type:1; member
736 GLenum prim_type; member
1312 ast_gs_input_layout(const struct YYLTYPE &locp, GLenum prim_type) in ast_gs_input_layout() argument
1313 : prim_type(prim_type) in ast_gs_input_layout()
1322 const GLenum prim_type;
/external/mesa3d/src/freedreno/.gitlab-ci/reference/
Des2gears-a320.log133 prim_type: DI_PT_POINTLIST_PSIZE (1)
428 prim_type: DI_PT_RECTLIST (8)
841 prim_type: DI_PT_TRISTRIP (6)
962 prim_type: DI_PT_TRISTRIP (6)
1010 prim_type: DI_PT_TRISTRIP (6)
1058 prim_type: DI_PT_TRISTRIP (6)
1106 prim_type: DI_PT_TRISTRIP (6)
1154 prim_type: DI_PT_TRISTRIP (6)
1202 prim_type: DI_PT_TRISTRIP (6)
1250 prim_type: DI_PT_TRISTRIP (6)
[all …]
/external/mesa3d/src/gallium/drivers/r600/sfn/
Dsfn_nir_lower_tess_io.cpp198 outer_tf_components(pipe_prim_type prim_type) in outer_tf_components() argument
200 switch (prim_type) { in outer_tf_components()
212 r600_lower_tess_io_impl(nir_builder *b, nir_instr *instr, enum pipe_prim_type prim_type) in r600_lower_tess_io_impl() argument
288 auto ncomps = outer_tf_components(prim_type); in r600_lower_tess_io_impl()
316 bool r600_lower_tess_io(nir_shader *shader, enum pipe_prim_type prim_type) in r600_lower_tess_io() argument
330 progress |= r600_lower_tess_io_impl(&b, instr, prim_type); in r600_lower_tess_io()
347 bool r600_append_tcs_TF_emission(nir_shader *shader, enum pipe_prim_type prim_type) { in r600_append_tcs_TF_emission() argument
370 auto outer_comps = outer_tf_components(prim_type); in r600_append_tcs_TF_emission()
415 if (prim_type == PIPE_PRIM_LINES) in r600_append_tcs_TF_emission()
Dsfn_nir.h113 bool r600_lower_tess_io(nir_shader *shader, enum pipe_prim_type prim_type);
114 bool r600_append_tcs_TF_emission(nir_shader *shader, enum pipe_prim_type prim_type);
/external/mesa3d/src/gallium/drivers/freedreno/
Dfreedreno_util.h107 static inline uint32_t DRAW(enum pc_di_primtype prim_type, in DRAW() argument
112 return (prim_type << 0) | in DRAW()
121 static inline uint32_t DRAW_A20X(enum pc_di_primtype prim_type, in DRAW_A20X() argument
128 return (prim_type << 0) | in DRAW_A20X()
/external/tensorflow/tensorflow/compiler/xla/tests/
Ddot_operation_test.cc243 auto prim_type = primitive_util::NativeToPrimitiveType<T>(); in TestImpl() local
244 Dot(Parameter(&builder, 0, ShapeUtil::MakeShape(prim_type, {2, 2}), "lhs"), in TestImpl()
245 Parameter(&builder, 1, ShapeUtil::MakeShape(prim_type, {2, 2}), "rhs")); in TestImpl()
353 auto prim_type = primitive_util::NativeToPrimitiveType<NativeT>(); in TestImpl() local
357 prim_type, {param.m, param.k}, in TestImpl()
362 prim_type, {param.k, param.n}, in TestImpl()
371 prim_type, {param.m, param.n}, in TestImpl()
529 auto prim_type = primitive_util::NativeToPrimitiveType<T>(); in TestImpl() local
530 Dot(Parameter(&builder, 0, ShapeUtil::MakeShape(prim_type, {2, 3}), "lhs"), in TestImpl()
531 Parameter(&builder, 1, ShapeUtil::MakeShape(prim_type, {3, 2}), "rhs")); in TestImpl()
[all …]
Dmatrix_ops_simple_test.cc195 auto prim_type = primitive_util::NativeToPrimitiveType<T>(); in TestImpl() local
197 ShapeUtil::MakeShape(prim_type, {lhs.height(), lhs.width()}); in TestImpl()
199 ShapeUtil::MakeShape(prim_type, {rhs.height(), rhs.width()}); in TestImpl()
/external/mesa3d/src/gallium/drivers/freedreno/a4xx/
Dfd4_draw.h38 static inline uint32_t DRAW4(enum pc_di_primtype prim_type, in DRAW4() argument
42 return CP_DRAW_INDX_OFFSET_0_PRIM_TYPE(prim_type) | in DRAW4()
/external/autotest/client/common_lib/cros/
Ddbus_send.py158 for prim_type, prefix in int_map.iteritems():
159 if isinstance(raw_arg, prim_type):
/external/mesa3d/src/gallium/auxiliary/draw/
Ddraw_pt_fetch_shade_pipeline.c380 prim_type(unsigned prim, unsigned flags) in prim_type() function
410 prim_info.prim = prim_type(fpme->input_prim, prim_flags); in fetch_pipeline_run()
438 prim_info.prim = prim_type(fpme->input_prim, prim_flags); in fetch_pipeline_linear_run()
469 prim_info.prim = prim_type(fpme->input_prim, prim_flags); in fetch_pipeline_linear_run_elts()
Ddraw_pt_fetch_shade_pipeline_llvm.c780 prim_type(unsigned prim, unsigned flags) in prim_type() function
810 prim_info.prim = prim_type(fpme->input_prim, prim_flags); in llvm_middle_end_run()
838 prim_info.prim = prim_type(fpme->input_prim, prim_flags); in llvm_middle_end_linear_run()
868 prim_info.prim = prim_type(fpme->input_prim, prim_flags); in llvm_middle_end_linear_run_elts()
/external/mesa3d/src/gallium/drivers/nouveau/nv50/
Dnv50_program.h97 uint8_t prim_type; /* point, line strip or tri strip */ member
/external/mesa3d/src/gallium/drivers/v3d/
Dv3d_context.c142 enum pipe_prim_type prim_type = u_base_prim_type(v3d->prim_mode); in v3d_update_primitive_counters() local
143 uint32_t num_verts = u_vertices_for_prims(prim_type, in v3d_update_primitive_counters()
/external/mesa3d/src/freedreno/decode/
Dcffdec.c1851 uint32_t prim_type = dwords[1] & 0x1f; in draw_indx_common() local
1856 primtype = rnn_enumname(rnn, "pc_di_primtype", prim_type); in draw_indx_common()
1862 prim_type); in draw_indx_common()
1971 uint32_t prim_type = dwords[0] & 0x1f; in cp_draw_indx_offset() local
1973 do_query(rnn_enumname(rnn, "pc_di_primtype", prim_type), num_indices); in cp_draw_indx_offset()
1984 uint32_t prim_type = dwords[0] & 0x1f; in cp_draw_indx_indirect() local
1987 do_query(rnn_enumname(rnn, "pc_di_primtype", prim_type), 0); in cp_draw_indx_indirect()
2008 uint32_t prim_type = dwords[0] & 0x1f; in cp_draw_indirect() local
2011 do_query(rnn_enumname(rnn, "pc_di_primtype", prim_type), 0); in cp_draw_indirect()
2023 uint32_t prim_type = dwords[0] & 0x1f; in cp_draw_indirect_multi() local
[all …]

12