Lines Matching refs:sync
443 memory_sync_info sync = get_sync_info(instr);
446 sync.storage = (storage_class)(sync.storage | storage_buffer);
447 sync.semantics =
448 (memory_semantics)((sync.semantics | semantic_private) & ~semantic_can_reorder);
450 return sync;
487 add_memory_event(memory_event_set* set, Instruction* instr, memory_sync_info* sync)
492 if (bar.sync.semantics & semantic_acquire)
493 set->bar_acquire |= bar.sync.storage;
494 if (bar.sync.semantics & semantic_release)
495 set->bar_release |= bar.sync.storage;
496 set->bar_classes |= bar.sync.storage;
501 if (!sync->storage)
504 if (sync->semantics & semantic_acquire)
505 set->access_acquire |= sync->storage;
506 if (sync->semantics & semantic_release)
507 set->access_release |= sync->storage;
509 if (!(sync->semantics & semantic_private)) {
510 if (sync->semantics & semantic_atomic)
511 set->access_atomic |= sync->storage;
513 set->access_relaxed |= sync->storage;
525 memory_sync_info sync = get_sync_info_with_hack(instr);
527 add_memory_event(&query->mem_events, instr, &sync);
529 if (!(sync.semantics & semantic_can_reorder)) {
530 unsigned storage = sync.storage;
582 memory_sync_info sync = get_sync_info_with_hack(instr);
583 add_memory_event(&instr_set, instr, &sync);
626 if ((sync.storage & aliasing_storage) && !(sync.semantics & semantic_can_reorder)) {
627 unsigned intersect = sync.storage & aliasing_storage;