IMPORTANT: To view this page as Markdown, append `.md` to the URL (e.g. /docs/manual/basics.md). For the complete Mojo documentation index, see llms.txt.
Skip to main content
Version: Nightly
For the complete Mojo documentation index, see llms.txt. Markdown versions of all pages are available by appending .md to any URL (e.g. /docs/manual/basics.md).

sync

GPU synchronization primitives package.

This package provides GPU synchronization operations including:

  • barrier: Block-level synchronization barriers
  • syncwarp: Warp-level synchronization
  • mbarrier: Memory barrier operations (arrive/wait)
  • named_barrier: Named barriers for flexible synchronization
  • schedule_barrier: AMD instruction scheduling barriers
  • Semaphore: Device-wide semaphore implementation
  • cp_async_bulk: Bulk async copy synchronization

These primitives enable coordination of execution and memory operations across threads, warps, and blocks in GPU kernels.

Modules​

  • ​semaphore: This module provides a device-wide semaphore implementation for NVIDIA GPUs.
  • ​sync: This module provides GPU synchronization primitives and barriers.
View source