/third_party/skia/third_party/externals/swiftshader/third_party/llvm-10.0/llvm/lib/Support/ |
H A D | APFloat.cpp | 35 llvm_unreachable("Unexpected semantics"); \ 53 /* Represents floating point arithmetic semantics. */ 67 /* Number of bits actually used in the semantics. */ 78 /* The IBM double-double semantics. Such a number consists of a pair of IEEE 89 /* These are legacy semantics for the fallback, inaccrurate implementation of 101 Currently, these semantics are used in the following way: 112 semantics. */ 131 llvm_unreachable("Unrecognised floating semantics"); in EnumToSemantics() 149 llvm_unreachable("Unknown floating semantics"); in SemanticsToEnum() 190 unsigned int APFloatBase::semanticsPrecision(const fltSemantics &semantics) { in semanticsPrecision() argument 194 semanticsMaxExponent(const fltSemantics &semantics) semanticsMaxExponent() argument 198 semanticsMinExponent(const fltSemantics &semantics) semanticsMinExponent() argument 201 semanticsSizeInBits(const fltSemantics &semantics) semanticsSizeInBits() argument [all...] |
/third_party/skia/third_party/externals/swiftshader/third_party/llvm-subzero/include/llvm/ADT/ |
H A D | APFloat.h | 67 /// full extended precision). Adding a new format that obeys IEEE semantics 207 /// semantics. 388 const fltSemantics &getSemantics() const { return *semantics; } in getSemantics() 395 /// magnitude in the current semantics. 399 /// magnitude in the current semantics. 476 /// semantics. 567 /// The semantics that this value obeys. 568 const fltSemantics *semantics; member in llvm::detail::final 597 // The interface and layout is designed for arbitray underlying semantics, 598 // though currently only PPCDoubleDouble semantics ar 660 const fltSemantics *semantics; global() member [all...] |
/third_party/mesa3d/src/compiler/nir/ |
H A D | nir_lower_passthrough_edgeflags.c | 62 nir_io_semantics semantics = {0}; in lower_impl() local 63 semantics.location = VARYING_SLOT_EDGE; in lower_impl() 64 semantics.num_slots = 1; in lower_impl() 69 .io_semantics = semantics, in lower_impl()
|
H A D | nir_gather_info.c | 474 nir_io_semantics semantics = nir_intrinsic_io_semantics(instr); in gather_intrinsic_info() local 476 if (semantics.location >= VARYING_SLOT_PATCH0 && in gather_intrinsic_info() 477 semantics.location <= VARYING_SLOT_PATCH31) { in gather_intrinsic_info() 485 semantics.location -= VARYING_SLOT_PATCH0; in gather_intrinsic_info() 488 if (semantics.location >= VARYING_SLOT_VAR0_16BIT && in gather_intrinsic_info() 489 semantics.location <= VARYING_SLOT_VAR15_16BIT) { in gather_intrinsic_info() 491 unsigned num_slots = (semantics.num_slots + semantics.high_16bits + 1) / 2; in gather_intrinsic_info() 493 BITFIELD_RANGE(semantics.location - VARYING_SLOT_VAR0_16BIT, num_slots); in gather_intrinsic_info() 495 slot_mask = BITFIELD64_RANGE(semantics in gather_intrinsic_info() [all...] |
H A D | nir_lower_clip.c | 100 nir_io_semantics semantics = { in store_clipdist_output() local 109 .io_semantics = semantics); in store_clipdist_output() 116 nir_io_semantics semantics = { in load_clipdist_input() local 130 .io_semantics = semantics); in load_clipdist_input() 136 .io_semantics = semantics); in load_clipdist_input()
|
H A D | nir_lower_io.c | 364 nir_io_semantics semantics = {0}; in emit_load() local 365 semantics.location = var->data.location; in emit_load() 366 semantics.num_slots = get_number_of_slots(state, var); in emit_load() 367 semantics.fb_fetch_output = var->data.fb_fetch_output; in emit_load() 368 semantics.medium_precision = in emit_load() 371 nir_intrinsic_set_io_semantics(load, semantics); in emit_load() 487 nir_io_semantics semantics = {0}; in emit_store() local 488 semantics.location = var->data.location; in emit_store() 489 semantics.num_slots = get_number_of_slots(state, var); in emit_store() 490 semantics in emit_store() 618 nir_io_semantics semantics = {0}; lower_interpolate_at() local [all...] |
H A D | nir_lower_memory_model.c | 26 * Replaces make availability/visible semantics on barriers with 159 unsigned semantics = nir_intrinsic_memory_semantics(intrin); in visit_instr() local 161 intrin, semantics & ~vis_avail_sem); in visit_instr()
|
/third_party/skia/third_party/externals/swiftshader/third_party/llvm-10.0/llvm/include/llvm/ADT/ |
H A D | APFloat.h | 30 llvm_unreachable("Unexpected semantics"); \ 77 /// full extended precision). Adding a new format that obeys IEEE semantics 236 /// semantics. 371 const fltSemantics &getSemantics() const { return *semantics; } in getSemantics() 378 /// magnitude in the current semantics. 382 /// magnitude in the current semantics. 465 /// semantics. 558 /// The semantics that this value obeys. 559 const fltSemantics *semantics; member in llvm::detail::final 588 // The interface and layout is designed for arbitray underlying semantics, 698 const fltSemantics *semantics; global() member [all...] |
/third_party/glslang/gtests/ |
H A D | TestFixture.h | 71 // Enum for shader compilation semantics. 184 // the target under the semantics conveyed via |controls|. Returns true 208 // |stage| into the target under the semantics specified via |controls|. 307 // |stage| into the target under the semantics specified via |controls|. 463 Semantics semantics, in loadFileCompileAndCheck() 482 EShMessages controls = DeriveOptions(source, semantics, target); in loadFileCompileAndCheck() 502 Semantics semantics, in loadFileCompileAndCheckWithOptions() 516 EShMessages controls = DeriveOptions(source, semantics, target); in loadFileCompileAndCheckWithOptions() 531 Semantics semantics, in loadFileCompileFlattenUniformsAndCheck() 543 const EShMessages controls = DeriveOptions(source, semantics, targe in loadFileCompileFlattenUniformsAndCheck() 460 loadFileCompileAndCheck(const std::string& testDir, const std::string& testName, Source source, Semantics semantics, glslang::EShTargetClientVersion clientTargetVersion, glslang::EShTargetLanguageVersion targetLanguageVersion, Target target, bool automap = true, const std::string& entryPointName=�, const std::string& baseDir=�, const bool enableOptimizer = false, const bool enableDebug = false, const bool enableNonSemanticShaderDebugInfo = false) loadFileCompileAndCheck() argument 499 loadFileCompileAndCheckWithOptions(const std::string &testDir, const std::string &testName, Source source, Semantics semantics, glslang::EShTargetClientVersion clientTargetVersion, glslang::EShTargetLanguageVersion targetLanguageVersion, Target target, bool automap = true, const std::string &entryPointName = �, const std::string &baseDir = �, const EShMessages additionalOptions = EShMessages::EShMsgDefault) loadFileCompileAndCheckWithOptions() argument 528 loadFileCompileFlattenUniformsAndCheck(const std::string& testDir, const std::string& testName, Source source, Semantics semantics, Target target, const std::string& entryPointName=�) loadFileCompileFlattenUniformsAndCheck() argument 555 loadFileCompileIoMapAndCheck(const std::string& testDir, const std::string& testName, Source source, Semantics semantics, Target target, const std::string& entryPointName, int baseSamplerBinding, int baseTextureBinding, int baseImageBinding, int baseUboBinding, int baseSsboBinding, bool autoMapBindings, bool flattenUniformArrays) loadFileCompileIoMapAndCheck() argument 592 loadFileCompileRemapAndCheck(const std::string& testDir, const std::string& testName, Source source, Semantics semantics, Target target, const std::string& entryPointName=�, const unsigned int remapOptions = spv::spirvbin_t::NONE) loadFileCompileRemapAndCheck() argument 619 loadFileRemapAndCheck(const std::string& testDir, const std::string& testName, Source source, Semantics semantics, Target target, const unsigned int remapOptions = spv::spirvbin_t::NONE) loadFileRemapAndCheck() argument 699 loadCompileUpgradeTextureToSampledTextureAndDropSamplersAndCheck(const std::string& testDir, const std::string& testName, Source source, Semantics semantics, Target target, const std::string& entryPointName = �) loadCompileUpgradeTextureToSampledTextureAndDropSamplersAndCheck() argument [all...] |
H A D | TestFixture.cpp | 85 EShMessages DeriveOptions(Source source, Semantics semantics, Target target) in DeriveOptions() argument 111 switch (semantics) { in DeriveOptions() 162 return std::make_pair(true, contents); // hopefully, c++11 move semantics optimizes the copy away. in ReadSpvBinaryFile()
|
H A D | GlslMapIO.FromFile.cpp | 50 Semantics semantics; member 239 Semantics semantics = GetParam().semantics; in TEST_P() local 241 const EShMessages controls = DeriveOptions(Source::GLSL, semantics, Target::BothASTAndSpv); in TEST_P() 346 // vulkan semantics
|
H A D | VkRelaxed.FromFile.cpp | 195 Semantics semantics = Semantics::Vulkan; in TEST_P() local 197 const EShMessages controls = DeriveOptions(Source::GLSL, semantics, Target::BothASTAndSpv); in TEST_P()
|
/third_party/skia/third_party/externals/angle2/src/common/spirv/ |
H A D | spirv_instruction_builder_autogen.h | 667 IdMemorySemantics semantics); 668 void WriteMemoryBarrier(Blob *blob, IdScope memory, IdMemorySemantics semantics); 674 IdMemorySemantics semantics); 678 IdMemorySemantics semantics, 685 IdMemorySemantics semantics, 701 IdMemorySemantics semantics); 707 IdMemorySemantics semantics); 713 IdMemorySemantics semantics, 720 IdMemorySemantics semantics, 727 IdMemorySemantics semantics, [all...] |
H A D | spirv_instruction_parser_autogen.h | 796 IdMemorySemantics *semantics); 799 IdMemorySemantics *semantics); 805 IdMemorySemantics *semantics); 809 IdMemorySemantics *semantics, 816 IdMemorySemantics *semantics, 832 IdMemorySemantics *semantics); 838 IdMemorySemantics *semantics); 844 IdMemorySemantics *semantics, 851 IdMemorySemantics *semantics, 858 IdMemorySemantics *semantics, [all...] |
H A D | spirv_instruction_builder_autogen.cpp | 2392 void WriteControlBarrier(Blob *blob, IdScope execution, IdScope memory, IdMemorySemantics semantics) in WriteControlBarrier() argument 2398 blob->push_back(semantics); in WriteControlBarrier() 2401 void WriteMemoryBarrier(Blob *blob, IdScope memory, IdMemorySemantics semantics) in WriteMemoryBarrier() argument 2406 blob->push_back(semantics); in WriteMemoryBarrier() 2414 IdMemorySemantics semantics) in WriteAtomicLoad() 2422 blob->push_back(semantics); in WriteAtomicLoad() 2428 IdMemorySemantics semantics, in WriteAtomicStore() 2435 blob->push_back(semantics); in WriteAtomicStore() 2444 IdMemorySemantics semantics, in WriteAtomicExchange() 2453 blob->push_back(semantics); in WriteAtomicExchange() 2409 WriteAtomicLoad(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics) WriteAtomicLoad() argument 2425 WriteAtomicStore(Blob *blob, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicStore() argument 2439 WriteAtomicExchange(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicExchange() argument 2479 WriteAtomicIIncrement(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics) WriteAtomicIIncrement() argument 2495 WriteAtomicIDecrement(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics) WriteAtomicIDecrement() argument 2511 WriteAtomicIAdd(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicIAdd() argument 2529 WriteAtomicISub(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicISub() argument 2547 WriteAtomicSMin(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicSMin() argument 2565 WriteAtomicUMin(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicUMin() argument 2583 WriteAtomicSMax(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicSMax() argument 2601 WriteAtomicUMax(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicUMax() argument 2619 WriteAtomicAnd(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicAnd() argument 2637 WriteAtomicOr(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicOr() argument 2655 WriteAtomicXor(Blob *blob, IdResultType idResultType, IdResult idResult, IdRef pointer, IdScope scope, IdMemorySemantics semantics, IdRef value) WriteAtomicXor() argument [all...] |
H A D | spirv_instruction_parser_autogen.cpp | 2885 IdMemorySemantics *semantics) in ParseControlBarrier() 2894 *semantics = IdMemorySemantics(_instruction[_o++]); in ParseControlBarrier() 2896 void ParseMemoryBarrier(const uint32_t *_instruction, IdScope *memory, IdMemorySemantics *semantics) in ParseMemoryBarrier() argument 2904 *semantics = IdMemorySemantics(_instruction[_o++]); in ParseMemoryBarrier() 2911 IdMemorySemantics *semantics) in ParseAtomicLoad() 2922 *semantics = IdMemorySemantics(_instruction[_o++]); in ParseAtomicLoad() 2927 IdMemorySemantics *semantics, in ParseAtomicStore() 2937 *semantics = IdMemorySemantics(_instruction[_o++]); in ParseAtomicStore() 2945 IdMemorySemantics *semantics, in ParseAtomicExchange() 2957 *semantics in ParseAtomicExchange() 2882 ParseControlBarrier(const uint32_t *_instruction, IdScope *execution, IdScope *memory, IdMemorySemantics *semantics) ParseControlBarrier() argument 2906 ParseAtomicLoad(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics) ParseAtomicLoad() argument 2924 ParseAtomicStore(const uint32_t *_instruction, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicStore() argument 2940 ParseAtomicExchange(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicExchange() argument 2984 ParseAtomicIIncrement(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics) ParseAtomicIIncrement() argument 3002 ParseAtomicIDecrement(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics) ParseAtomicIDecrement() argument 3020 ParseAtomicIAdd(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicIAdd() argument 3040 ParseAtomicISub(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicISub() argument 3060 ParseAtomicSMin(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicSMin() argument 3080 ParseAtomicUMin(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicUMin() argument 3100 ParseAtomicSMax(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicSMax() argument 3120 ParseAtomicUMax(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicUMax() argument 3140 ParseAtomicAnd(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicAnd() argument 3160 ParseAtomicOr(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicOr() argument 3180 ParseAtomicXor(const uint32_t *_instruction, IdResultType *idResultType, IdResult *idResult, IdRef *pointer, IdScope *scope, IdMemorySemantics *semantics, IdRef *value) ParseAtomicXor() argument [all...] |
/third_party/mesa3d/src/gallium/drivers/r600/sfn/ |
H A D | sfn_shader_fs.cpp | 466 auto semantics = nir_intrinsic_io_semantics(&intr); in emit_export_pixel() local 470 switch (semantics.location) { in emit_export_pixel() 488 if (semantics.location == FRAG_RESULT_COLOR || in emit_export_pixel() 489 (semantics.location >= FRAG_RESULT_DATA0 && in emit_export_pixel() 490 semantics.location <= FRAG_RESULT_DATA7)) { in emit_export_pixel() 500 unsigned location = (m_dual_source_blend && (semantics.location == FRAG_RESULT_COLOR) in emit_export_pixel() 501 ? semantics.dual_source_blend_index : driver_location) + k - m_depth_exports; in emit_export_pixel() 521 if (semantics.location == FRAG_RESULT_COLOR && in emit_export_pixel() 522 semantics.dual_source_blend_index > 0) in emit_export_pixel() 532 } else if (semantics in emit_export_pixel() [all...] |
/third_party/mesa3d/src/amd/compiler/ |
H A D | aco_scheduler.cpp | 447 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)) { 626 if ((sync.storage & aliasing_storage) && !(sync.semantics [all...] |
/third_party/node/deps/v8/src/compiler/ |
H A D | simplified-lowering-verifier.cc | 242 if (const Operator* semantics = p.semantics()) { in VisitNode() 243 switch (semantics->opcode()) { in VisitNode()
|
H A D | common-operator.h | 35 // The semantics of IrOpcode::kBranch changes throughout the pipeline, and in 36 // particular is not the same before SimplifiedLowering (JS semantics) and after 37 // (machine branch semantics). Some passes are applied both before and after 429 explicit SLVerifierHintParameters(const Operator* semantics, in SLVerifierHintParameters() argument 431 : semantics_(semantics), override_output_type_(override_output_type) {} in SLVerifierHintParameters() 433 const Operator* semantics() const { return semantics_; } in semantics() function in v8::internal::compiler::final 476 const Operator* semantics,
|
/third_party/mesa3d/src/amd/common/ |
H A D | ac_nir_lower_tess_io_to_mem.c | 429 nir_io_semantics semantics = nir_intrinsic_io_semantics(intrin); in lower_hs_output_store() local 432 bool is_tess_factor = semantics.location == VARYING_SLOT_TESS_LEVEL_INNER || in lower_hs_output_store() 433 semantics.location == VARYING_SLOT_TESS_LEVEL_OUTER; in lower_hs_output_store() 450 if (semantics.location == VARYING_SLOT_TESS_LEVEL_INNER) in lower_hs_output_store() 452 else if (semantics.location == VARYING_SLOT_TESS_LEVEL_OUTER) in lower_hs_output_store()
|
/third_party/mesa3d/src/gallium/auxiliary/nir/ |
H A D | nir_to_tgsi.c | 669 nir_io_semantics semantics = nir_intrinsic_io_semantics(instr); in ntt_output_decl() local 677 tgsi_get_gl_frag_result_semantic(semantics.location, in ntt_output_decl() 679 semantic_index += semantics.dual_source_blend_index; in ntt_output_decl() 681 switch (semantics.location) { in ntt_output_decl() 696 ntt_get_gl_varying_semantic(c, semantics.location, in ntt_output_decl() 702 uint32_t gs_streams = semantics.gs_streams; in ntt_output_decl() 711 /* This bit is lost in the i/o semantics, but it's unused in in-tree in ntt_output_decl() 714 bool invariant = semantics.invariant; in ntt_output_decl() 722 semantics.num_slots, in ntt_output_decl() 2151 nir_io_semantics semantics in ntt_emit_load_input() local 2283 nir_io_semantics semantics = nir_intrinsic_io_semantics(instr); ntt_emit_load_output() local 3279 nir_io_semantics semantics = nir_intrinsic_io_semantics(second); nir_to_tgsi_lower_64bit_intrinsic() local 3658 nir_io_semantics semantics = { nir_lower_primid_sysval_to_input_lower() local [all...] |
/third_party/mesa3d/src/compiler/spirv/ |
H A D | spirv_to_nir.c | 2294 SpvMemorySemanticsMask semantics, in vtn_split_barrier_semantics() 2298 /* For memory semantics embedded in operations, we split them into up to in vtn_split_barrier_semantics() 2312 semantics & (SpvMemorySemanticsAcquireMask | in vtn_split_barrier_semantics() 2322 vtn_warn("Multiple memory ordering semantics specified, " in vtn_split_barrier_semantics() 2328 semantics & (SpvMemorySemanticsMakeAvailableMask | in vtn_split_barrier_semantics() 2332 semantics & (SpvMemorySemanticsUniformMemoryMask | in vtn_split_barrier_semantics() 2341 semantics & ~(order_semantics | av_vis_semantics | storage_semantics | in vtn_split_barrier_semantics() 2345 vtn_warn("Ignoring unhandled memory semantics: %u\n", other_semantics); in vtn_split_barrier_semantics() 2351 * semantics will not be reordered after the Store. in vtn_split_barrier_semantics() 2360 * associated with a Load. All the operations with a matching semantics in vtn_split_barrier_semantics() 2293 vtn_split_barrier_semantics(struct vtn_builder *b, SpvMemorySemanticsMask semantics, SpvMemorySemanticsMask *before, SpvMemorySemanticsMask *after) vtn_split_barrier_semantics() argument 2377 vtn_mem_semantics_to_nir_mem_semantics(struct vtn_builder *b, SpvMemorySemanticsMask semantics) vtn_mem_semantics_to_nir_mem_semantics() argument 2439 vtn_mem_semantics_to_nir_var_modes(struct vtn_builder *b, SpvMemorySemanticsMask semantics) vtn_mem_semantics_to_nir_var_modes() argument 2519 vtn_emit_scoped_control_barrier(struct vtn_builder *b, SpvScope exec_scope, SpvScope mem_scope, SpvMemorySemanticsMask semantics) vtn_emit_scoped_control_barrier() argument 2540 vtn_emit_scoped_memory_barrier(struct vtn_builder *b, SpvScope scope, SpvMemorySemanticsMask semantics) vtn_emit_scoped_memory_barrier() argument 3239 SpvMemorySemanticsMask semantics = 0; vtn_handle_image() local 3679 SpvMemorySemanticsMask semantics = 0; vtn_handle_atomics() local 4120 vtn_emit_memory_barrier(struct vtn_builder *b, SpvScope scope, SpvMemorySemanticsMask semantics) vtn_emit_memory_barrier() argument 4223 SpvMemorySemanticsMask semantics = vtn_constant_uint(b, w[2]); vtn_handle_barrier() local [all...] |
/third_party/skia/third_party/externals/swiftshader/src/Pipeline/ |
H A D | SpirvShaderControlFlow.cpp | 625 auto semantics = spv::MemorySemanticsMask(GetConstScalarInt(insn.word(3))); in EmitControlBarrier() local 628 Fence(semantics); in EmitControlBarrier() 716 void SpirvShader::Fence(spv::MemorySemanticsMask semantics) const in Fence() 718 if(semantics == spv::MemorySemanticsMaskNone) in Fence() 722 rr::Fence(MemoryOrder(semantics)); in Fence()
|
/third_party/mesa3d/src/gallium/drivers/zink/nir_to_spirv/ |
H A D | spirv_builder.h | 183 SpvMemorySemanticsMask semantics, SpvId object); 451 spirv_builder_emit_memory_barrier(struct spirv_builder *b, SpvScope scope, SpvMemorySemanticsMask semantics); 454 spirv_builder_emit_control_barrier(struct spirv_builder *b, SpvScope scope, SpvScope mem_scope, SpvMemorySemanticsMask semantics);
|