tilelang.cuda.language.cluster
==============================

.. py:module:: tilelang.cuda.language.cluster


Functions
---------

.. autoapisummary::

   tilelang.cuda.language.cluster.cluster_arrive_relaxed
   tilelang.cuda.language.cluster.cluster_arrive
   tilelang.cuda.language.cluster.cluster_wait
   tilelang.cuda.language.cluster.cluster_sync
   tilelang.cuda.language.cluster.block_rank_in_cluster
   tilelang.cuda.language.cluster.clc_try_cancel
   tilelang.cuda.language.cluster.clc_try_cancel_multicast
   tilelang.cuda.language.cluster.clc_is_canceled
   tilelang.cuda.language.cluster.clc_get_first_ctaid_x
   tilelang.cuda.language.cluster.clc_get_first_ctaid_y
   tilelang.cuda.language.cluster.clc_get_first_ctaid_z


Module Contents
---------------

.. py:function:: cluster_arrive_relaxed()

   Issue barrier.cluster.arrive.relaxed.aligned.


.. py:function:: cluster_arrive()

   Issue barrier.cluster.arrive.aligned.


.. py:function:: cluster_wait()

   Issue barrier.cluster.wait.aligned.


.. py:function:: cluster_sync()

   Issue cluster barrier arrive + wait (full synchronization).


.. py:function:: block_rank_in_cluster()

   Return the 1-D rank of the calling CTA within its cluster (%%cluster_ctarank).


.. py:function:: clc_try_cancel(result, mbarrier)

   Issue a single-CTA cluster launch control query.


.. py:function:: clc_try_cancel_multicast(result, mbarrier)

   Issue a cluster-wide multicast cluster launch control query.


.. py:function:: clc_is_canceled(result)

   Return 1 when the CLC query successfully canceled a future launch.


.. py:function:: clc_get_first_ctaid_x(result)

   Return the x coordinate of the first CTA in a successful CLC response.


.. py:function:: clc_get_first_ctaid_y(result)

   Return the y coordinate of the first CTA in a successful CLC response.


.. py:function:: clc_get_first_ctaid_z(result)

   Return the z coordinate of the first CTA in a successful CLC response.