Searched refs:semantics (Results 1 - 25 of 51) sorted by relevance

123

/xsrc/external/mit/MesaLib/dist/src/compiler/nir/
H A Dnir_lower_passthrough_edgeflags.c62 nir_io_semantics semantics = {0}; local in function:lower_impl
63 semantics.location = VARYING_SLOT_EDGE;
64 semantics.num_slots = 1;
69 .io_semantics = semantics,
H A Dnir_gather_info.c430 nir_io_semantics semantics = nir_intrinsic_io_semantics(instr); local in function:gather_intrinsic_info
432 if (semantics.location >= VARYING_SLOT_PATCH0 &&
433 semantics.location <= VARYING_SLOT_PATCH31) {
441 semantics.location -= VARYING_SLOT_PATCH0;
444 if (semantics.location >= VARYING_SLOT_VAR0_16BIT &&
445 semantics.location <= VARYING_SLOT_VAR15_16BIT) {
447 unsigned num_slots = (semantics.num_slots + semantics.high_16bits + 1) / 2;
449 BITFIELD_RANGE(semantics.location - VARYING_SLOT_VAR0_16BIT, num_slots);
451 slot_mask = BITFIELD64_RANGE(semantics
[all...]
H A Dnir_lower_clip.c98 nir_io_semantics semantics = { local in function:store_clipdist_output
106 .io_semantics = semantics);
113 nir_io_semantics semantics = { local in function:load_clipdist_input
121 .io_semantics = semantics);
H A Dnir_lower_memory_model.c26 * Replaces make availability/visible semantics on barriers with
159 unsigned semantics = nir_intrinsic_memory_semantics(intrin); local in function:visit_instr
161 intrin, semantics & ~vis_avail_sem);
H A Dnir_lower_io.c315 nir_io_semantics semantics = {0}; local in function:emit_load
316 semantics.location = var->data.location;
317 semantics.num_slots = get_number_of_slots(state, var);
318 semantics.fb_fetch_output = var->data.fb_fetch_output;
319 semantics.medium_precision =
322 nir_intrinsic_set_io_semantics(load, semantics);
438 nir_io_semantics semantics = {0}; local in function:emit_store
439 semantics.location = var->data.location;
440 semantics.num_slots = get_number_of_slots(state, var);
441 semantics
567 nir_io_semantics semantics = {0}; local in function:lower_interpolate_at
[all...]
H A Dnir_print.c913 nir_memory_semantics semantics = nir_intrinsic_memory_semantics(instr); local in function:print_intrinsic_instr
915 switch (semantics & (NIR_MEMORY_ACQUIRE | NIR_MEMORY_RELEASE)) {
921 if (semantics & (NIR_MEMORY_MAKE_AVAILABLE)) fprintf(fp, "|AVAILABLE");
922 if (semantics & (NIR_MEMORY_MAKE_VISIBLE)) fprintf(fp, "|VISIBLE");
/xsrc/external/mit/MesaLib/dist/src/gtest/include/gtest/internal/custom/
H A DREADME.md12 `testing::TempDir` for semantics and signature.
/xsrc/external/mit/MesaLib/dist/src/amd/compiler/
H A Daco_dead_code_analysis.cpp91 return !(get_sync_info(instr).semantics & (semantic_volatile | semantic_acqrel));
H A Daco_scheduler.cpp447 sync.semantics =
448 (memory_semantics)((sync.semantics | semantic_private) & ~semantic_can_reorder);
492 if (bar.sync.semantics & semantic_acquire)
494 if (bar.sync.semantics & semantic_release)
504 if (sync->semantics & semantic_acquire)
506 if (sync->semantics & semantic_release)
509 if (!(sync->semantics & semantic_private)) {
510 if (sync->semantics & semantic_atomic)
529 if (!(sync.semantics & semantic_can_reorder)) {
624 if ((sync.storage & aliasing_storage) && !(sync.semantics
[all...]
H A Daco_insert_waitcnt.cpp305 perform_barrier(wait_ctx& ctx, wait_imm& imm, memory_sync_info sync, unsigned semantics) argument
309 if ((sync.semantics & semantics) && sync.scope > subgroup_scope) {
477 if (sync.storage & (1 << i) && !(sync.semantics & semantic_private)) {
H A Daco_ir.h183 memory_sync_info() : storage(storage_none), semantics(semantic_none), scope(scope_invocation) {}
185 : storage((storage_class)storage_), semantics((memory_semantics)semantics_), scope(scope_)
189 memory_semantics semantics : 8; member in struct:aco::memory_sync_info
194 return storage == rhs.storage && semantics == rhs.semantics && scope == rhs.scope;
199 if (semantics & semantic_acqrel)
203 return (!storage || (semantics & semantic_can_reorder)) && !(semantics & semantic_volatile);
H A Daco_print_ir.cpp233 fprintf(output, " semantics:");
268 print_semantics(sync.semantics, output);
/xsrc/external/mit/MesaLib/dist/src/compiler/spirv/
H A Dspirv_to_nir.c2236 SpvMemorySemanticsMask semantics,
2240 /* For memory semantics embedded in operations, we split them into up to
2254 semantics & (SpvMemorySemanticsAcquireMask |
2264 vtn_warn("Multiple memory ordering semantics specified, "
2270 semantics & (SpvMemorySemanticsMakeAvailableMask |
2274 semantics & (SpvMemorySemanticsUniformMemoryMask |
2283 semantics & ~(order_semantics | av_vis_semantics | storage_semantics |
2287 vtn_warn("Ignoring unhandled memory semantics: %u\n", other_semantics);
2293 * semantics will not be reordered after the Store.
2302 * associated with a Load. All the operations with a matching semantics
2235 vtn_split_barrier_semantics(struct vtn_builder * b,SpvMemorySemanticsMask semantics,SpvMemorySemanticsMask * before,SpvMemorySemanticsMask * after) argument
2319 vtn_mem_semantics_to_nir_mem_semantics(struct vtn_builder * b,SpvMemorySemanticsMask semantics) argument
2381 vtn_mem_semantics_to_nir_var_modes(struct vtn_builder * b,SpvMemorySemanticsMask semantics) argument
2461 vtn_emit_scoped_control_barrier(struct vtn_builder * b,SpvScope exec_scope,SpvScope mem_scope,SpvMemorySemanticsMask semantics) argument
2482 vtn_emit_scoped_memory_barrier(struct vtn_builder * b,SpvScope scope,SpvMemorySemanticsMask semantics) argument
3180 SpvMemorySemanticsMask semantics = 0; local in function:vtn_handle_image
3611 SpvMemorySemanticsMask semantics = 0; local in function:vtn_handle_atomics
4048 vtn_emit_memory_barrier(struct vtn_builder * b,SpvScope scope,SpvMemorySemanticsMask semantics) argument
4151 SpvMemorySemanticsMask semantics = vtn_constant_uint(b, w[2]); local in function:vtn_handle_barrier
[all...]
H A Dvtn_private.h1031 SpvMemorySemanticsMask semantics);
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/r600/sfn/
H A Dsfn_shader_fragment.cpp913 auto semantics = nir_intrinsic_io_semantics(instr); local in function:r600::FragmentShaderFromNir::emit_export_pixel
916 switch (semantics.location) {
939 if (semantics.location == FRAG_RESULT_COLOR ||
940 (semantics.location >= FRAG_RESULT_DATA0 &&
941 semantics.location <= FRAG_RESULT_DATA7)) {
944 unsigned location = (m_dual_source_blend && (semantics.location == FRAG_RESULT_COLOR)
945 ? semantics.dual_source_blend_index : driver_location) + k - m_depth_exports;
968 } else if (semantics.location == FRAG_RESULT_DEPTH ||
969 semantics.location == FRAG_RESULT_STENCIL ||
970 semantics
[all...]
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/zink/nir_to_spirv/
H A Dspirv_builder.h183 SpvMemorySemanticsMask semantics, SpvId object);
441 spirv_builder_emit_memory_barrier(struct spirv_builder *b, SpvScope scope, SpvMemorySemanticsMask semantics);
444 spirv_builder_emit_control_barrier(struct spirv_builder *b, SpvScope scope, SpvScope mem_scope, SpvMemorySemanticsMask semantics);
H A Dspirv_builder.c439 SpvMemorySemanticsMask semantics, SpvId object)
445 spirv_buffer_emit_word(&b->instructions, spirv_builder_const_uint(b, 32, semantics));
1509 spirv_builder_emit_memory_barrier(struct spirv_builder *b, SpvScope scope, SpvMemorySemanticsMask semantics) argument
1514 spirv_buffer_emit_word(&b->instructions, spirv_builder_const_uint(b, 32, semantics));
1518 spirv_builder_emit_control_barrier(struct spirv_builder *b, SpvScope scope, SpvScope mem_scope, SpvMemorySemanticsMask semantics) argument
1524 spirv_buffer_emit_word(&b->instructions, spirv_builder_const_uint(b, 32, semantics));
438 spirv_builder_emit_atomic_store(struct spirv_builder * b,SpvId pointer,SpvScope scope,SpvMemorySemanticsMask semantics,SpvId object) argument
/xsrc/external/mit/MesaLib/dist/src/amd/common/
H A Dac_nir_lower_tess_io_to_mem.c394 nir_io_semantics semantics = nir_intrinsic_io_semantics(intrin); local in function:lower_hs_output_store
397 bool is_tess_factor = semantics.location == VARYING_SLOT_TESS_LEVEL_INNER ||
398 semantics.location == VARYING_SLOT_TESS_LEVEL_OUTER;
414 if (semantics.location == VARYING_SLOT_TESS_LEVEL_INNER)
416 else if (semantics.location == VARYING_SLOT_TESS_LEVEL_OUTER)
/xsrc/external/mit/MesaLib/dist/src/gallium/auxiliary/nir/
H A Dnir_to_tgsi.c192 nir_io_semantics semantics = nir_intrinsic_io_semantics(instr); local in function:ntt_output_decl
200 tgsi_get_gl_frag_result_semantic(semantics.location,
202 semantic_index += semantics.dual_source_blend_index;
204 switch (semantics.location) {
219 ntt_get_gl_varying_semantic(c, semantics.location,
225 uint32_t gs_streams = semantics.gs_streams;
234 /* This bit is lost in the i/o semantics, but it's unused in in-tree
245 semantics.num_slots,
1675 nir_io_semantics semantics = nir_intrinsic_io_semantics(instr); local in function:ntt_emit_load_input
1680 for (int i = 1; i < semantics
2646 nir_io_semantics semantics = nir_intrinsic_io_semantics(second); local in function:nir_to_tgsi_lower_64bit_intrinsic
3029 nir_io_semantics semantics = { local in function:nir_lower_primid_sysval_to_input_lower
[all...]
/xsrc/external/mit/MesaLib/dist/docs/relnotes/
H A D13.0.1.rst139 - radeonsi: fix BFE/BFI lowering for GLSL semantics
H A D7.9.2.rst228 - glsl: Track variable usage, use that to enforce semantics
/xsrc/external/mit/MesaLib.old/dist/src/gallium/docs/source/
H A Dresources.rst102 2D surface with OpenGL GL_TEXTURE_RECTANGLE semantics.
/xsrc/external/mit/MesaLib/dist/docs/gallium/
H A Dresources.rst102 2D surface with OpenGL GL_TEXTURE_RECTANGLE semantics.
/xsrc/external/mit/MesaLib.old/dist/src/compiler/spirv/
H A Dspirv_to_nir.c2824 SpvMemorySemanticsMask semantics = w[5];
3291 SpvMemorySemanticsMask semantics)
3300 if (!(semantics & all_memory_semantics))
3317 if ((semantics & all_memory_semantics) == all_memory_semantics) {
3323 uint32_t bits = semantics;
3389 SpvMemorySemanticsMask semantics = vtn_constant_uint(b, w[2]); local in function:vtn_handle_barrier
3390 vtn_emit_memory_barrier(b, scope, semantics);
3290 vtn_emit_memory_barrier(struct vtn_builder * b,SpvScope scope,SpvMemorySemanticsMask semantics) argument
/xsrc/external/mit/libdrm/dist/man/
H A Ddrm-memory.7.rst138 the semantics (and if it applies, the syntax) that is shared between all

Completed in 47 milliseconds

123