Ubuntu Manpages

Graph Management

\brief graph management functions of the CUDA runtime API (cuda_runtime_api.h)

This section describes the graph management functions of CUDA runtime application programming interface.

cudaError_t cudaGraphAddChildGraphNode (cudaGraphNode_t * pGraphNode, cudaGraph_t graph, const cudaGraphNode_t * pDependencies, size_t numDependencies, cudaGraph_t childGraph)

Creates a new node which executes an embedded graph, and adds it to graph with numDependencies dependencies specified via pDependencies. It is possible for numDependencies to be 0, in which case the node will be placed at the root of the graph. pDependencies may not have any duplicate entries. A handle to the new node will be returned in pGraphNode.

The node executes an embedded child graph. The child graph is cloned in this call.

Parameters:

pGraphNode - Returns newly created node
graph - Graph to which to add the node
pDependencies - Dependencies of the node
numDependencies - Number of dependencies
childGraph - The graph to clone into this node

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphChildGraphNodeGetGraph, cudaGraphCreate, cudaGraphDestroyNode, cudaGraphAddEmptyNode, cudaGraphAddKernelNode, cudaGraphAddHostNode, cudaGraphAddMemcpyNode, cudaGraphAddMemsetNode, cudaGraphClone

cudaError_t cudaGraphAddDependencies (cudaGraph_t graph, const cudaGraphNode_t * from, const cudaGraphNode_t * to, size_t numDependencies)

The number of dependencies to be added is defined by numDependencies Elements in pFrom and pTo at corresponding indices define a dependency. Each node in pFrom and pTo must belong to graph.

If numDependencies is 0, elements in pFrom and pTo will be ignored. Specifying an existing dependency will return an error.

Parameters:

graph - Graph to which dependencies are added
from - Array of nodes that provide the dependencies
to - Array of dependent nodes
numDependencies - Number of dependencies to be added

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphRemoveDependencies, cudaGraphGetEdges, cudaGraphNodeGetDependencies, cudaGraphNodeGetDependentNodes

cudaError_t cudaGraphAddEmptyNode (cudaGraphNode_t * pGraphNode, cudaGraph_t graph, const cudaGraphNode_t * pDependencies, size_t numDependencies)

Creates a new node which performs no operation, and adds it to graph with numDependencies dependencies specified via pDependencies. It is possible for numDependencies to be 0, in which case the node will be placed at the root of the graph. pDependencies may not have any duplicate entries. A handle to the new node will be returned in pGraphNode.

An empty node performs no operation during execution, but can be used for transitive ordering. For example, a phased execution graph with 2 groups of n nodes with a barrier between them can be represented using an empty node and 2*n dependency edges, rather than no empty node and n^2 dependency edges.

Parameters:

pGraphNode - Returns newly created node
graph - Graph to which to add the node
pDependencies - Dependencies of the node
numDependencies - Number of dependencies

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

See also:

cudaGraphCreate, cudaGraphDestroyNode, cudaGraphAddChildGraphNode, cudaGraphAddKernelNode, cudaGraphAddHostNode, cudaGraphAddMemcpyNode, cudaGraphAddMemsetNode

cudaError_t cudaGraphAddHostNode (cudaGraphNode_t * pGraphNode, cudaGraph_t graph, const cudaGraphNode_t * pDependencies, size_t numDependencies, const struct cudaHostNodeParams * pNodeParams)

Creates a new CPU execution node and adds it to graph with numDependencies dependencies specified via pDependencies and arguments specified in pNodeParams. It is possible for numDependencies to be 0, in which case the node will be placed at the root of the graph. pDependencies may not have any duplicate entries. A handle to the new node will be returned in pGraphNode.

When the graph is launched, the node will invoke the specified CPU function. Host nodes are not supported under MPS with pre-Volta GPUs.

Parameters:

pGraphNode - Returns newly created node
graph - Graph to which to add the node
pDependencies - Dependencies of the node
numDependencies - Number of dependencies
pNodeParams - Parameters for the host node

Returns:

cudaSuccess, cudaErrorNotSupported, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaLaunchHostFunc, cudaGraphHostNodeGetParams, cudaGraphHostNodeSetParams, cudaGraphCreate, cudaGraphDestroyNode, cudaGraphAddChildGraphNode, cudaGraphAddEmptyNode, cudaGraphAddKernelNode, cudaGraphAddMemcpyNode, cudaGraphAddMemsetNode

cudaError_t cudaGraphAddKernelNode (cudaGraphNode_t * pGraphNode, cudaGraph_t graph, const cudaGraphNode_t * pDependencies, size_t numDependencies, const struct cudaKernelNodeParams * pNodeParams)

Creates a new kernel execution node and adds it to graph with numDependencies dependencies specified via pDependencies and arguments specified in pNodeParams. It is possible for numDependencies to be 0, in which case the node will be placed at the root of the graph. pDependencies may not have any duplicate entries. A handle to the new node will be returned in pGraphNode.

The cudaKernelNodeParams structure is defined as:

  struct cudaKernelNodeParams
  {
      void* func;
      dim3 gridDim;
      dim3 blockDim;
      unsigned int sharedMemBytes;
      void **kernelParams;
      void **extra;
  };

When the graph is launched, the node will invoke kernel func on a (gridDim.x x gridDim.y x gridDim.z) grid of blocks. Each block contains (blockDim.x x blockDim.y x blockDim.z) threads.

sharedMem sets the amount of dynamic shared memory that will be available to each thread block.

Kernel parameters to func can be specified in one of two ways:

1) Kernel parameters can be specified via kernelParams. If the kernel has N parameters, then kernelParams needs to be an array of N pointers. Each pointer, from kernelParams[0] to kernelParams[N-1], points to the region of memory from which the actual parameter will be copied. The number of kernel parameters and their offsets and sizes do not need to be specified as that information is retrieved directly from the kernel's image.

2) Kernel parameters can also be packaged by the application into a single buffer that is passed in via extra. This places the burden on the application of knowing each kernel parameter's size and alignment/padding within the buffer. The extra parameter exists to allow this function to take additional less commonly used arguments. extra specifies a list of names of extra settings and their corresponding values. Each extra setting name is immediately followed by the corresponding value. The list must be terminated with either NULL or CU_LAUNCH_PARAM_END.

  • CU_LAUNCH_PARAM_END, which indicates the end of the extra array;
  • CU_LAUNCH_PARAM_BUFFER_POINTER, which specifies that the next value in extra will be a pointer to a buffer containing all the kernel parameters for launching kernel func;
  • CU_LAUNCH_PARAM_BUFFER_SIZE, which specifies that the next value in extra will be a pointer to a size_t containing the size of the buffer specified with CU_LAUNCH_PARAM_BUFFER_POINTER;

The error cudaErrorInvalidValue will be returned if kernel parameters are specified with both kernelParams and extra (i.e. both kernelParams and extra are non-NULL).

The kernelParams or extra array, as well as the argument values it points to, are copied during this call.

Note:

Kernels launched using graphs must not use texture and surface references. Reading or writing through any texture or surface reference is undefined behavior. This restriction does not apply to texture and surface objects.

Parameters:

pGraphNode - Returns newly created node
graph - Graph to which to add the node
pDependencies - Dependencies of the node
numDependencies - Number of dependencies
pNodeParams - Parameters for the GPU execution node

Returns:

cudaSuccess, cudaErrorInvalidValue, cudaErrorInvalidDeviceFunction

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaLaunchKernel, cudaGraphKernelNodeGetParams, cudaGraphKernelNodeSetParams, cudaGraphCreate, cudaGraphDestroyNode, cudaGraphAddChildGraphNode, cudaGraphAddEmptyNode, cudaGraphAddHostNode, cudaGraphAddMemcpyNode, cudaGraphAddMemsetNode

cudaError_t cudaGraphAddMemcpyNode (cudaGraphNode_t * pGraphNode, cudaGraph_t graph, const cudaGraphNode_t * pDependencies, size_t numDependencies, const struct cudaMemcpy3DParms * pCopyParams)

Creates a new memcpy node and adds it to graph with numDependencies dependencies specified via pDependencies. It is possible for numDependencies to be 0, in which case the node will be placed at the root of the graph. pDependencies may not have any duplicate entries. A handle to the new node will be returned in pGraphNode.

When the graph is launched, the node will perform the memcpy described by pCopyParams. See cudaMemcpy3D() for a description of the structure and its restrictions.

Memcpy nodes have some additional restrictions with regards to managed memory, if the system contains at least one device which has a zero value for the device attribute cudaDevAttrConcurrentManagedAccess.

Parameters:

pGraphNode - Returns newly created node
graph - Graph to which to add the node
pDependencies - Dependencies of the node
numDependencies - Number of dependencies
pCopyParams - Parameters for the memory copy

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaMemcpy3D, cudaGraphMemcpyNodeGetParams, cudaGraphMemcpyNodeSetParams, cudaGraphCreate, cudaGraphDestroyNode, cudaGraphAddChildGraphNode, cudaGraphAddEmptyNode, cudaGraphAddKernelNode, cudaGraphAddHostNode, cudaGraphAddMemsetNode

cudaError_t cudaGraphAddMemsetNode (cudaGraphNode_t * pGraphNode, cudaGraph_t graph, const cudaGraphNode_t * pDependencies, size_t numDependencies, const struct cudaMemsetParams * pMemsetParams)

Creates a new memset node and adds it to graph with numDependencies dependencies specified via pDependencies. It is possible for numDependencies to be 0, in which case the node will be placed at the root of the graph. pDependencies may not have any duplicate entries. A handle to the new node will be returned in pGraphNode.

The element size must be 1, 2, or 4 bytes. When the graph is launched, the node will perform the memset described by pMemsetParams.

Parameters:

pGraphNode - Returns newly created node
graph - Graph to which to add the node
pDependencies - Dependencies of the node
numDependencies - Number of dependencies
pMemsetParams - Parameters for the memory set

Returns:

cudaSuccess, cudaErrorInvalidValue, cudaErrorInvalidDevice

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaMemset2D, cudaGraphMemsetNodeGetParams, cudaGraphMemsetNodeSetParams, cudaGraphCreate, cudaGraphDestroyNode, cudaGraphAddChildGraphNode, cudaGraphAddEmptyNode, cudaGraphAddKernelNode, cudaGraphAddHostNode, cudaGraphAddMemcpyNode

cudaError_t cudaGraphChildGraphNodeGetGraph (cudaGraphNode_t node, cudaGraph_t * pGraph)

Gets a handle to the embedded graph in a child graph node. This call does not clone the graph. Changes to the graph will be reflected in the node, and the node retains ownership of the graph.

Parameters:

node - Node to get the embedded graph for
pGraph - Location to store a handle to the graph

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphAddChildGraphNode, cudaGraphNodeFindInClone

cudaError_t cudaGraphClone (cudaGraph_t * pGraphClone, cudaGraph_t originalGraph)

This function creates a copy of originalGraph and returns it in pGraphClone. All parameters are copied into the cloned graph. The original graph may be modified after this call without affecting the clone.

Child graph nodes in the original graph are recursively copied into the clone.

Parameters:

pGraphClone - Returns newly created cloned graph
originalGraph - Graph to clone

Returns:

cudaSuccess, cudaErrorInvalidValue, cudaErrorMemoryAllocation

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphCreate, cudaGraphNodeFindInClone

cudaError_t cudaGraphCreate (cudaGraph_t * pGraph, unsigned int flags)

Creates an empty graph, which is returned via pGraph.

Parameters:

pGraph - Returns newly created graph
flags - Graph creation flags, must be 0

Returns:

cudaSuccess, cudaErrorInvalidValue, cudaErrorMemoryAllocation

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphAddChildGraphNode, cudaGraphAddEmptyNode, cudaGraphAddKernelNode, cudaGraphAddHostNode, cudaGraphAddMemcpyNode, cudaGraphAddMemsetNode, cudaGraphInstantiate, cudaGraphDestroy, cudaGraphGetNodes, cudaGraphGetRootNodes, cudaGraphGetEdges, cudaGraphClone

cudaError_t cudaGraphDestroy (cudaGraph_t graph)

Destroys the graph specified by graph, as well as all of its nodes.

Parameters:

graph - Graph to destroy

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphCreate

cudaError_t cudaGraphDestroyNode (cudaGraphNode_t node)

Removes node from its graph. This operation also severs any dependencies of other nodes on node and vice versa.

Parameters:

node - Node to remove

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphAddChildGraphNode, cudaGraphAddEmptyNode, cudaGraphAddKernelNode, cudaGraphAddHostNode, cudaGraphAddMemcpyNode, cudaGraphAddMemsetNode

cudaError_t cudaGraphExecDestroy (cudaGraphExec_t graphExec)

Destroys the executable graph specified by graphExec.

Parameters:

graphExec - Executable graph to destroy

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphInstantiate, cudaGraphLaunch

cudaError_t cudaGraphExecKernelNodeSetParams (cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const struct cudaKernelNodeParams * pNodeParams)

Sets the parameters of a kernel node in an executable graph hGraphExec. The node is identified by the corresponding node node in the non-executable graph, from which the executable graph was instantiated.

node must not have been removed from the original graph. The func field of nodeParams cannot be modified and must match the original value. All other values can be modified.

The modifications take effect at the next launch of hGraphExec. Already enqueued or running launches of hGraphExec are not affected by this call. node is also not modified by this call.

Parameters:

hGraphExec - The executable graph in which to set the specified node
node - kernel node from the graph from which graphExec was instantiated
pNodeParams - Updated Parameters to set

Returns:

cudaSuccess, cudaErrorInvalidValue,

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphAddKernelNode, cudaGraphKernelNodeSetParams, cudaGraphInstantiate

cudaError_t cudaGraphGetEdges (cudaGraph_t graph, cudaGraphNode_t * from, cudaGraphNode_t * to, size_t * numEdges)

Returns a list of graph's dependency edges. Edges are returned via corresponding indices in from and to; that is, the node in to[i] has a dependency on the node in from[i]. from and to may both be NULL, in which case this function only returns the number of edges in numEdges. Otherwise, numEdges entries will be filled in. If numEdges is higher than the actual number of edges, the remaining entries in from and to will be set to NULL, and the number of edges actually returned will be written to numEdges.

Parameters:

graph - Graph to get the edges from
from - Location to return edge endpoints
to - Location to return edge endpoints
numEdges - See description

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphGetNodes, cudaGraphGetRootNodes, cudaGraphAddDependencies, cudaGraphRemoveDependencies, cudaGraphNodeGetDependencies, cudaGraphNodeGetDependentNodes

cudaError_t cudaGraphGetNodes (cudaGraph_t graph, cudaGraphNode_t * nodes, size_t * numNodes)

Returns a list of graph's nodes. nodes may be NULL, in which case this function will return the number of nodes in numNodes. Otherwise, numNodes entries will be filled in. If numNodes is higher than the actual number of nodes, the remaining entries in nodes will be set to NULL, and the number of nodes actually obtained will be returned in numNodes.

Parameters:

graph - Graph to query
nodes - Pointer to return the nodes
numNodes - See description

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphCreate, cudaGraphGetRootNodes, cudaGraphGetEdges, cudaGraphNodeGetType, cudaGraphNodeGetDependencies, cudaGraphNodeGetDependentNodes

cudaError_t cudaGraphGetRootNodes (cudaGraph_t graph, cudaGraphNode_t * pRootNodes, size_t * pNumRootNodes)

Returns a list of graph's root nodes. pRootNodes may be NULL, in which case this function will return the number of root nodes in pNumRootNodes. Otherwise, pNumRootNodes entries will be filled in. If pNumRootNodes is higher than the actual number of root nodes, the remaining entries in pRootNodes will be set to NULL, and the number of nodes actually obtained will be returned in pNumRootNodes.

Parameters:

graph - Graph to query
pRootNodes - Pointer to return the root nodes
pNumRootNodes - See description

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphCreate, cudaGraphGetNodes, cudaGraphGetEdges, cudaGraphNodeGetType, cudaGraphNodeGetDependencies, cudaGraphNodeGetDependentNodes

cudaError_t cudaGraphHostNodeGetParams (cudaGraphNode_t node, struct cudaHostNodeParams * pNodeParams)

Returns the parameters of host node node in pNodeParams.

Parameters:

node - Node to get the parameters for
pNodeParams - Pointer to return the parameters

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaLaunchHostFunc, cudaGraphAddHostNode, cudaGraphHostNodeSetParams

cudaError_t cudaGraphHostNodeSetParams (cudaGraphNode_t node, const struct cudaHostNodeParams * pNodeParams)

Sets the parameters of host node node to nodeParams.

Parameters:

node - Node to set the parameters for
pNodeParams - Parameters to copy

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaLaunchHostFunc, cudaGraphAddHostNode, cudaGraphHostNodeGetParams

cudaError_t cudaGraphInstantiate (cudaGraphExec_t * pGraphExec, cudaGraph_t graph, cudaGraphNode_t * pErrorNode, char * pLogBuffer, size_t bufferSize)

Instantiates graph as an executable graph. The graph is validated for any structural constraints or intra-node constraints which were not previously validated. If instantiation is successful, a handle to the instantiated graph is returned in pGraphExec.

If there are any errors, diagnostic information may be returned in pErrorNode and pLogBuffer. This is the primary way to inspect instantiation errors. The output will be null terminated unless the diagnostics overflow the buffer. In this case, they will be truncated, and the last byte can be inspected to determine if truncation occurred.

Parameters:

pGraphExec - Returns instantiated graph
graph - Graph to instantiate
pErrorNode - In case of an instantiation error, this may be modified to indicate a node contributing to the error
pLogBuffer - A character buffer to store diagnostic messages
bufferSize - Size of the log buffer in bytes

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphCreate, cudaGraphLaunch, cudaGraphExecDestroy

cudaError_t cudaGraphKernelNodeGetParams (cudaGraphNode_t node, struct cudaKernelNodeParams * pNodeParams)

Returns the parameters of kernel node node in pNodeParams. The kernelParams or extra array returned in pNodeParams, as well as the argument values it points to, are owned by the node. This memory remains valid until the node is destroyed or its parameters are modified, and should not be modified directly. Use cudaGraphKernelNodeSetParams to update the parameters of this node.

The params will contain either kernelParams or extra, according to which of these was most recently set on the node.

Parameters:

node - Node to get the parameters for
pNodeParams - Pointer to return the parameters

Returns:

cudaSuccess, cudaErrorInvalidValue, cudaErrorInvalidDeviceFunction

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaLaunchKernel, cudaGraphAddKernelNode, cudaGraphKernelNodeSetParams

cudaError_t cudaGraphKernelNodeSetParams (cudaGraphNode_t node, const struct cudaKernelNodeParams * pNodeParams)

Sets the parameters of kernel node node to pNodeParams.

Parameters:

node - Node to set the parameters for
pNodeParams - Parameters to copy

Returns:

cudaSuccess, cudaErrorInvalidValue, cudaErrorInvalidResourceHandle, cudaErrorMemoryAllocation

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaLaunchKernel, cudaGraphAddKernelNode, cudaGraphKernelNodeGetParams

cudaError_t cudaGraphLaunch (cudaGraphExec_t graphExec, cudaStream_t stream)

Executes graphExec in stream. Only one instance of graphExec may be executing at a time. Each launch is ordered behind both any previous work in stream and any previous launches of graphExec. To execute a graph concurrently, it must be instantiated multiple times into multiple executable graphs.

Parameters:

graphExec - Executable graph to launch
stream - Stream in which to launch the graph

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphInstantiate, cudaGraphExecDestroy

cudaError_t cudaGraphMemcpyNodeGetParams (cudaGraphNode_t node, struct cudaMemcpy3DParms * pNodeParams)

Returns the parameters of memcpy node node in pNodeParams.

Parameters:

node - Node to get the parameters for
pNodeParams - Pointer to return the parameters

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaMemcpy3D, cudaGraphAddMemcpyNode, cudaGraphMemcpyNodeSetParams

cudaError_t cudaGraphMemcpyNodeSetParams (cudaGraphNode_t node, const struct cudaMemcpy3DParms * pNodeParams)

Sets the parameters of memcpy node node to pNodeParams.

Parameters:

node - Node to set the parameters for
pNodeParams - Parameters to copy

Returns:

cudaSuccess, cudaErrorInvalidValue,

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaMemcpy3D, cudaGraphAddMemcpyNode, cudaGraphMemcpyNodeGetParams

cudaError_t cudaGraphMemsetNodeGetParams (cudaGraphNode_t node, struct cudaMemsetParams * pNodeParams)

Returns the parameters of memset node node in pNodeParams.

Parameters:

node - Node to get the parameters for
pNodeParams - Pointer to return the parameters

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaMemset2D, cudaGraphAddMemsetNode, cudaGraphMemsetNodeSetParams

cudaError_t cudaGraphMemsetNodeSetParams (cudaGraphNode_t node, const struct cudaMemsetParams * pNodeParams)

Sets the parameters of memset node node to pNodeParams.

Parameters:

node - Node to set the parameters for
pNodeParams - Parameters to copy

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaMemset2D, cudaGraphAddMemsetNode, cudaGraphMemsetNodeGetParams

cudaError_t cudaGraphNodeFindInClone (cudaGraphNode_t * pNode, cudaGraphNode_t originalNode, cudaGraph_t clonedGraph)

This function returns the node in clonedGraph corresponding to originalNode in the original graph.

clonedGraph must have been cloned from originalGraph via cudaGraphClone. originalNode must have been in originalGraph at the time of the call to cudaGraphClone, and the corresponding cloned node in clonedGraph must not have been removed. The cloned node is then returned via pClonedNode.

Parameters:

pNode - Returns handle to the cloned node
originalNode - Handle to the original node
clonedGraph - Cloned graph to query

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphClone

cudaError_t cudaGraphNodeGetDependencies (cudaGraphNode_t node, cudaGraphNode_t * pDependencies, size_t * pNumDependencies)

Returns a list of node's dependencies. pDependencies may be NULL, in which case this function will return the number of dependencies in pNumDependencies. Otherwise, pNumDependencies entries will be filled in. If pNumDependencies is higher than the actual number of dependencies, the remaining entries in pDependencies will be set to NULL, and the number of nodes actually obtained will be returned in pNumDependencies.

Parameters:

node - Node to query
pDependencies - Pointer to return the dependencies
pNumDependencies - See description

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphNodeGetDependentNodes, cudaGraphGetNodes, cudaGraphGetRootNodes, cudaGraphGetEdges, cudaGraphAddDependencies, cudaGraphRemoveDependencies

cudaError_t cudaGraphNodeGetDependentNodes (cudaGraphNode_t node, cudaGraphNode_t * pDependentNodes, size_t * pNumDependentNodes)

Returns a list of node's dependent nodes. pDependentNodes may be NULL, in which case this function will return the number of dependent nodes in pNumDependentNodes. Otherwise, pNumDependentNodes entries will be filled in. If pNumDependentNodes is higher than the actual number of dependent nodes, the remaining entries in pDependentNodes will be set to NULL, and the number of nodes actually obtained will be returned in pNumDependentNodes.

Parameters:

node - Node to query
pDependentNodes - Pointer to return the dependent nodes
pNumDependentNodes - See description

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphNodeGetDependencies, cudaGraphGetNodes, cudaGraphGetRootNodes, cudaGraphGetEdges, cudaGraphAddDependencies, cudaGraphRemoveDependencies

cudaError_t cudaGraphNodeGetType (cudaGraphNode_t node, enum cudaGraphNodeType * pType)

Returns the node type of node in pType.

Parameters:

node - Node to query
pType - Pointer to return the node type

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphGetNodes, cudaGraphGetRootNodes, cudaGraphChildGraphNodeGetGraph, cudaGraphKernelNodeGetParams, cudaGraphKernelNodeSetParams, cudaGraphHostNodeGetParams, cudaGraphHostNodeSetParams, cudaGraphMemcpyNodeGetParams, cudaGraphMemcpyNodeSetParams, cudaGraphMemsetNodeGetParams, cudaGraphMemsetNodeSetParams

cudaError_t cudaGraphRemoveDependencies (cudaGraph_t graph, const cudaGraphNode_t * from, const cudaGraphNode_t * to, size_t numDependencies)

The number of pDependencies to be removed is defined by numDependencies. Elements in pFrom and pTo at corresponding indices define a dependency. Each node in pFrom and pTo must belong to graph.

If numDependencies is 0, elements in pFrom and pTo will be ignored. Specifying a non-existing dependency will return an error.

Parameters:

graph - Graph from which to remove dependencies
from - Array of nodes that provide the dependencies
to - Array of dependent nodes
numDependencies - Number of dependencies to be removed

Returns:

cudaSuccess, cudaErrorInvalidValue

Note:

Graph objects are not threadsafe. .

Note that this function may also return error codes from previous, asynchronous launches.

See also:

cudaGraphAddDependencies, cudaGraphGetEdges, cudaGraphNodeGetDependencies, cudaGraphNodeGetDependentNodes

Generated automatically by Doxygen from the source code.