<!DOCTYPE html
PUBLIC "-//W3C//DTD XHTML 1.0 Transitional//EN" "http://www.w3.org/TR/xhtml1/DTD/xhtml1-transitional.dtd">
<html xmlns="http://www.w3.org/1999/xhtml" lang="en-us" xml:lang="en-us">
<head>
<meta http-equiv="Content-Type" content="text/html; charset=utf-8"></meta>
<meta http-equiv="X-UA-Compatible" content="IE=edge"></meta>
<meta name="copyright" content="(C) Copyright 2005"></meta>
<meta name="DC.rights.owner" content="(C) Copyright 2005"></meta>
<meta name="DC.Type" content="cppModule"></meta>
<meta name="DC.Title" content="Thread Management [DEPRECATED]"></meta>
<meta name="abstract" content=""></meta>
<meta name="description" content=""></meta>
<meta name="DC.Format" content="XHTML"></meta>
<meta name="DC.Identifier" content="group__CUDART__THREAD__DEPRECATED"></meta>
<link rel="stylesheet" type="text/css" href="../common/formatting/commonltr.css"></link>
<link rel="stylesheet" type="text/css" href="../common/formatting/site.css"></link>
<title>CUDA Runtime API :: CUDA Toolkit Documentation</title>
<!--[if lt IE 9]>
<script src="../common/formatting/html5shiv-printshiv.min.js"></script>
<![endif]-->
<script type="text/javascript" charset="utf-8" src="../common/formatting/jquery.min.js"></script>
<script type="text/javascript" charset="utf-8" src="../common/formatting/jquery.ba-hashchange.min.js"></script>
<link rel="canonical" href="http://docs.nvidia.com/cuda/cuda-runtime-api/index.html"></link>
<link rel="stylesheet" type="text/css" href="../common/formatting/qwcode.highlight.css"></link>
</head>
<body>
<article id="contents">
<div id="breadcrumbs"><a href="group__CUDART__DEVICE.html" shape="rect">< Previous</a> | <a href="group__CUDART__ERROR.html" shape="rect">Next ></a></div>
<div id="release-info">CUDA Runtime API
(<a href="../../pdf/CUDA_Runtime_API.pdf">PDF</a>)
-
CUDA Toolkit v5.5
(<a href="https://developer.nvidia.com/cuda-toolkit-archive">older</a>)
-
Last updated
July 19, 2013
-
<a href="mailto:cudatools@nvidia.com?subject=CUDA Tools Documentation Feedback: cuda-runtime-api">Send Feedback</a></div>
<div class="topic reference apiRef apiPackage cppModule" id="group__CUDART__THREAD__DEPRECATED"><a name="group__CUDART__THREAD__DEPRECATED" shape="rect">
<!-- --></a><h2 class="topictitle2 cppModule">2.2. Thread Management [DEPRECATED]</h2>
<div class="section">
<p>This section describes deprecated thread management functions of the CUDA runtime application programming interface. </p>
</div>
<h3 class="fake_sectiontitle member_header">Functions</h3>
<dl class="members">
<dt><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" shape="rect">cudaThreadExit</a> ( void ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Exit and clean up from CUDA launches. </span></dd>
<dt><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__THREAD__DEPRECATED_1g7a82ef85e4f7e0cff0a84b2f7f6bc63a" shape="rect">cudaThreadGetCacheConfig</a> ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" title="" shape="rect">cudaFuncCache *</a>*<span> </span><span class="keyword keyword apiItemName">pCacheConfig</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Returns the preferred cache configuration for the current device. </span></dd>
<dt><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__THREAD__DEPRECATED_1gfd87d16d2bbf4bc41a892f3f75bac5e0" shape="rect">cudaThreadGetLimit</a> ( size_t*<span> </span><span class="keyword keyword apiItemName">pValue</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" title="" shape="rect">cudaLimit</a><span> </span><span class="keyword keyword apiItemName">limit</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Returns resource limits. </span></dd>
<dt><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__THREAD__DEPRECATED_1g27d0f538b3018142bf04deae7f02c49e" shape="rect">cudaThreadSetCacheConfig</a> ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" title="" shape="rect">cudaFuncCache</a><span> </span><span class="keyword keyword apiItemName">cacheConfig</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Sets the preferred cache configuration for the current device. </span></dd>
<dt><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__THREAD__DEPRECATED_1gd636fe22576028cdf3d2c271b544b316" shape="rect">cudaThreadSetLimit</a> ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" title="" shape="rect">cudaLimit</a><span> </span><span class="keyword keyword apiItemName">limit</span>, size_t<span> </span><span class="keyword keyword apiItemName">value</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Set resource limits. </span></dd>
<dt><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__THREAD__DEPRECATED_1g6e0c5163e6f959b56b6ae2eaa8483576" shape="rect">cudaThreadSynchronize</a> ( void ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Wait for compute device to finish. </span></dd>
</dl>
<div class="description">
<h3 class="sectiontitle">Functions</h3>
<dl class="description">
<dt class="description"><a name="group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" id="group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" shape="rect">
<!-- --></a><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaThreadExit ( void ) </span></dt>
<dd class="description">
<div class="section">Exit and clean up from CUDA launches. </div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a></p>
</div>
<div class="section">
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000001" shape="rect">Deprecated</a></h6>
<p>Note that this function is deprecated because its name does not reflect its behavior. Its functionality is identical to the
non-deprecated function <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gdcc2c6f914eb9461565b12648faa5e28" title="Destroy all allocations and reset all state on the current device in the current process." shape="rect">cudaDeviceReset()</a>, which should be used instead.
</p>
<h6 class="description_header">Description</h6>
<p class="p">Explicitly destroys all cleans up all resources associated with the current device in the current process. Any subsequent
API call to this device will reinitialize the device.
</p>
<p class="p">Note that this function will reset the device immediately. It is the caller's responsibility to ensure that the device is
not being accessed by any other host threads from the process when this function is called.
</p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gdcc2c6f914eb9461565b12648faa5e28" title="Destroy all allocations and reset all state on the current device in the current process." shape="rect">cudaDeviceReset</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__THREAD__DEPRECATED_1g7a82ef85e4f7e0cff0a84b2f7f6bc63a" id="group__CUDART__THREAD__DEPRECATED_1g7a82ef85e4f7e0cff0a84b2f7f6bc63a" shape="rect">
<!-- --></a><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaThreadGetCacheConfig ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" title="" shape="rect">cudaFuncCache *</a>*<span> </span><span class="keyword keyword apiItemName">pCacheConfig</span> ) </span></dt>
<dd class="description">
<div class="section">Returns the preferred cache configuration for the current device. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">pCacheConfig</span></tt></dt>
<dd>- Returned cache configuration</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038ce7993a88ecf2c57b8102d55d997a18c" shape="rect">cudaErrorInitializationError</a></p>
</div>
<div class="section">
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000005" shape="rect">Deprecated</a></h6>
<p>Note that this function is deprecated because its name does not reflect its behavior. Its functionality is identical to the
non-deprecated function <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g91d4f0ad53af9cef174b764598444349" title="Returns the preferred cache configuration for the current device." shape="rect">cudaDeviceGetCacheConfig()</a>, which should be used instead.
</p>
<h6 class="description_header">Description</h6>
<p class="p">On devices where the L1 cache and shared memory use the same hardware resources, this returns through <tt class="ph tt code">pCacheConfig</tt> the preferred cache configuration for the current device. This is only a preference. The runtime will use the requested configuration
if possible, but it is free to choose a different configuration if required to execute functions.
</p>
<p class="p">This will return a <tt class="ph tt code">pCacheConfig</tt> of <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b3b4b8c65376ce1ca107be413e15981bc" shape="rect">cudaFuncCachePreferNone</a> on devices where the size of the L1 cache and shared memory are fixed.
</p>
<p class="p">The supported cache configurations are:
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b3b4b8c65376ce1ca107be413e15981bc" shape="rect">cudaFuncCachePreferNone</a>: no preference for shared memory or L1 (default)
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b84725d25c531f9bafc61ae329afe5b2b" shape="rect">cudaFuncCachePreferShared</a>: prefer larger shared memory and smaller L1 cache
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b8ecb48ccbc2230c81528a2c7c695100e" shape="rect">cudaFuncCachePreferL1</a>: prefer larger L1 cache and smaller shared memory
</p>
</li>
</ul>
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g91d4f0ad53af9cef174b764598444349" title="Returns the preferred cache configuration for the current device." shape="rect">cudaDeviceGetCacheConfig</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__THREAD__DEPRECATED_1gfd87d16d2bbf4bc41a892f3f75bac5e0" id="group__CUDART__THREAD__DEPRECATED_1gfd87d16d2bbf4bc41a892f3f75bac5e0" shape="rect">
<!-- --></a><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaThreadGetLimit ( size_t*<span> </span><span class="keyword keyword apiItemName">pValue</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" title="" shape="rect">cudaLimit</a><span> </span><span class="keyword keyword apiItemName">limit</span> ) </span></dt>
<dd class="description">
<div class="section">Returns resource limits. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">pValue</span></tt></dt>
<dd>- Returned size in bytes of limit</dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">limit</span></tt></dt>
<dd>- Limit to query </dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038c3b950b6f8668f7282fae25bfcefd13a" shape="rect">cudaErrorUnsupportedLimit</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a></p>
</div>
<div class="section">
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000004" shape="rect">Deprecated</a></h6>
<p>Note that this function is deprecated because its name does not reflect its behavior. Its functionality is identical to the
non-deprecated function <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g879c2d7d3be80c4afc6e4d14674fee93" title="Returns resource limits." shape="rect">cudaDeviceGetLimit()</a>, which should be used instead.
</p>
<h6 class="description_header">Description</h6>
<p class="p">Returns in <tt class="ph tt code">*pValue</tt> the current size of <tt class="ph tt code">limit</tt>. The supported <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" shape="rect">cudaLimit</a> values are:
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc93651fc8f54e641c9b133f1b57703d22ce656" shape="rect">cudaLimitStackSize</a>: stack size of each GPU thread;
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365123b80a6221a6853e918c2816bb76742c" shape="rect">cudaLimitPrintfFifoSize</a>: size of the shared FIFO used by the printf() and fprintf() device system calls.
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc93651b399716bf0a592bc42055473c1273881" shape="rect">cudaLimitMallocHeapSize</a>: size of the heap used by the malloc() and free() device system calls;
</p>
</li>
</ul>
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g879c2d7d3be80c4afc6e4d14674fee93" title="Returns resource limits." shape="rect">cudaDeviceGetLimit</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__THREAD__DEPRECATED_1g27d0f538b3018142bf04deae7f02c49e" id="group__CUDART__THREAD__DEPRECATED_1g27d0f538b3018142bf04deae7f02c49e" shape="rect">
<!-- --></a><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaThreadSetCacheConfig ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" title="" shape="rect">cudaFuncCache</a><span> </span><span class="keyword keyword apiItemName">cacheConfig</span> ) </span></dt>
<dd class="description">
<div class="section">Sets the preferred cache configuration for the current device. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">cacheConfig</span></tt></dt>
<dd>- Requested cache configuration</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038ce7993a88ecf2c57b8102d55d997a18c" shape="rect">cudaErrorInitializationError</a></p>
</div>
<div class="section">
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000006" shape="rect">Deprecated</a></h6>
<p>Note that this function is deprecated because its name does not reflect its behavior. Its functionality is identical to the
non-deprecated function <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gac27b566beee1aa9175373bb9e29b8d1" title="Sets the preferred cache configuration for the current device." shape="rect">cudaDeviceSetCacheConfig()</a>, which should be used instead.
</p>
<h6 class="description_header">Description</h6>
<p class="p">On devices where the L1 cache and shared memory use the same hardware resources, this sets through <tt class="ph tt code">cacheConfig</tt> the preferred cache configuration for the current device. This is only a preference. The runtime will use the requested configuration
if possible, but it is free to choose a different configuration if required to execute the function. Any function preference
set via <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g4f35d04be20a41c5df96613a748eecc1" title="Sets the preferred cache configuration for a device function." shape="rect">cudaFuncSetCacheConfig ( C API)</a> or cudaFuncSetCacheConfig (C++ API) will be preferred over this device-wide setting. Setting the device-wide cache configuration
to <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b3b4b8c65376ce1ca107be413e15981bc" shape="rect">cudaFuncCachePreferNone</a> will cause subsequent kernel launches to prefer to not change the cache configuration unless required to launch the kernel.
</p>
<p class="p">This setting does nothing on devices where the size of the L1 cache and shared memory are fixed.</p>
<p class="p">Launching a kernel with a different preference than the most recent preference setting may insert a device-side synchronization
point.
</p>
<p class="p">The supported cache configurations are:
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b3b4b8c65376ce1ca107be413e15981bc" shape="rect">cudaFuncCachePreferNone</a>: no preference for shared memory or L1 (default)
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b84725d25c531f9bafc61ae329afe5b2b" shape="rect">cudaFuncCachePreferShared</a>: prefer larger shared memory and smaller L1 cache
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b8ecb48ccbc2230c81528a2c7c695100e" shape="rect">cudaFuncCachePreferL1</a>: prefer larger L1 cache and smaller shared memory
</p>
</li>
</ul>
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gac27b566beee1aa9175373bb9e29b8d1" title="Sets the preferred cache configuration for the current device." shape="rect">cudaDeviceSetCacheConfig</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__THREAD__DEPRECATED_1gd636fe22576028cdf3d2c271b544b316" id="group__CUDART__THREAD__DEPRECATED_1gd636fe22576028cdf3d2c271b544b316" shape="rect">
<!-- --></a><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaThreadSetLimit ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" title="" shape="rect">cudaLimit</a><span> </span><span class="keyword keyword apiItemName">limit</span>, size_t<span> </span><span class="keyword keyword apiItemName">value</span> ) </span></dt>
<dd class="description">
<div class="section">Set resource limits. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">limit</span></tt></dt>
<dd>- Limit to set </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">value</span></tt></dt>
<dd>- Size in bytes of limit</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038c3b950b6f8668f7282fae25bfcefd13a" shape="rect">cudaErrorUnsupportedLimit</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a></p>
</div>
<div class="section">
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000003" shape="rect">Deprecated</a></h6>
<p>Note that this function is deprecated because its name does not reflect its behavior. Its functionality is identical to the
non-deprecated function <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gb8a22e29cc297634b0702db0b69f59e7" title="Set resource limits." shape="rect">cudaDeviceSetLimit()</a>, which should be used instead.
</p>
<h6 class="description_header">Description</h6>
<p class="p">Setting <tt class="ph tt code">limit</tt> to <tt class="ph tt code">value</tt> is a request by the application to update the current limit maintained by the device. The driver is free to modify the requested
value to meet h/w requirements (this could be clamping to minimum or maximum values, rounding up to nearest element size,
etc). The application can use <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1gfd87d16d2bbf4bc41a892f3f75bac5e0" title="Returns resource limits." shape="rect">cudaThreadGetLimit()</a> to find out exactly what the limit has been set to.
</p>
<p class="p">Setting each <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" shape="rect">cudaLimit</a> has its own specific restrictions, so each is discussed here.
</p>
<p class="p">
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc93651fc8f54e641c9b133f1b57703d22ce656" shape="rect">cudaLimitStackSize</a> controls the stack size of each GPU thread. This limit is only applicable to devices of compute capability 2.0 and higher.
Attempting to set this limit on devices of compute capability less than 2.0 will result in the error <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038c3b950b6f8668f7282fae25bfcefd13a" shape="rect">cudaErrorUnsupportedLimit</a> being returned.
</p>
</li>
</ul>
</p>
<p class="p">
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365123b80a6221a6853e918c2816bb76742c" shape="rect">cudaLimitPrintfFifoSize</a> controls the size of the shared FIFO used by the printf() and fprintf() device system calls. Setting <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365123b80a6221a6853e918c2816bb76742c" shape="rect">cudaLimitPrintfFifoSize</a> must be performed before launching any kernel that uses the printf() or fprintf() device system calls, otherwise <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a> will be returned. This limit is only applicable to devices of compute capability 2.0 and higher. Attempting to set this limit
on devices of compute capability less than 2.0 will result in the error <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038c3b950b6f8668f7282fae25bfcefd13a" shape="rect">cudaErrorUnsupportedLimit</a> being returned.
</p>
</li>
</ul>
</p>
<p class="p">
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc93651b399716bf0a592bc42055473c1273881" shape="rect">cudaLimitMallocHeapSize</a> controls the size of the heap used by the malloc() and free() device system calls. Setting <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc93651b399716bf0a592bc42055473c1273881" shape="rect">cudaLimitMallocHeapSize</a> must be performed before launching any kernel that uses the malloc() or free() device system calls, otherwise <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a> will be returned. This limit is only applicable to devices of compute capability 2.0 and higher. Attempting to set this limit
on devices of compute capability less than 2.0 will result in the error <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038c3b950b6f8668f7282fae25bfcefd13a" shape="rect">cudaErrorUnsupportedLimit</a> being returned.
</p>
</li>
</ul>
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gb8a22e29cc297634b0702db0b69f59e7" title="Set resource limits." shape="rect">cudaDeviceSetLimit</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__THREAD__DEPRECATED_1g6e0c5163e6f959b56b6ae2eaa8483576" id="group__CUDART__THREAD__DEPRECATED_1g6e0c5163e6f959b56b6ae2eaa8483576" shape="rect">
<!-- --></a><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaThreadSynchronize ( void ) </span></dt>
<dd class="description">
<div class="section">Wait for compute device to finish. </div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a></p>
</div>
<div class="section">
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000002" shape="rect">Deprecated</a></h6>
<p>Note that this function is deprecated because its name does not reflect its behavior. Its functionality is similar to the
non-deprecated function <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g32bdc6229081137acd3cba5da2897779" title="Wait for compute device to finish." shape="rect">cudaDeviceSynchronize()</a>, which should be used instead.
</p>
<h6 class="description_header">Description</h6>
<p class="p">Blocks until the device has completed all preceding requested tasks. <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1g6e0c5163e6f959b56b6ae2eaa8483576" title="Wait for compute device to finish." shape="rect">cudaThreadSynchronize()</a> returns an error if one of the preceding tasks has failed. If the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" shape="rect">cudaDeviceScheduleBlockingSync</a> flag was set for this device, the host thread will block until the device has finished its work.
</p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g32bdc6229081137acd3cba5da2897779" title="Wait for compute device to finish." shape="rect">cudaDeviceSynchronize</a></p>
<p class="p"></p>
</div>
</dd>
</dl>
</div>
</div>
<hr id="contents-end"></hr>
<div id="breadcrumbs"><a href="group__CUDART__DEVICE.html" shape="rect">< Previous</a> | <a href="group__CUDART__ERROR.html" shape="rect">Next ></a></div>
<div id="release-info">CUDA Runtime API
(<a href="../../pdf/CUDA_Runtime_API.pdf">PDF</a>)
-
CUDA Toolkit v5.5
(<a href="https://developer.nvidia.com/cuda-toolkit-archive">older</a>)
-
Last updated
July 19, 2013
-
<a href="mailto:cudatools@nvidia.com?subject=CUDA Tools Documentation Feedback: cuda-runtime-api">Send Feedback</a></div>
</article>
<header id="header"><span id="company">NVIDIA</span><span id="site-title">CUDA Toolkit Documentation</span><form id="search" method="get" action="search">
<input type="text" name="search-text"></input><fieldset id="search-location">
<legend>Search In:</legend>
<label><input type="radio" name="search-type" value="site"></input>Entire Site</label>
<label><input type="radio" name="search-type" value="document"></input>Just This Document</label></fieldset>
<button type="reset">clear search</button>
<button id="submit" type="submit">search</button></form>
</header>
<nav id="site-nav">
<div class="category closed"><span class="twiddle">▷</span><a href="../index.html" title="The root of the site.">CUDA Toolkit</a></div>
<ul class="closed">
<li><a href="../cuda-toolkit-release-notes/index.html" title="The Release Notes for the CUDA Toolkit from v4.0 to today.">Release Notes</a></li>
<li><a href="../eula/index.html" title="The End User License Agreements for the NVIDIA CUDA Toolkit, the NVIDIA CUDA Samples, the NVIDIA Display Driver, and NVIDIA NSight (Visual Studio Edition).">EULA</a></li>
<li><a href="../cuda-getting-started-guide-for-linux/index.html" title="This guide discusses how to install and check for correct operation of the CUDA Development Tools on GNU/Linux systems.">Getting Started Linux</a></li>
<li><a href="../cuda-getting-started-guide-for-mac-os-x/index.html" title="This guide discusses how to install and check for correct operation of the CUDA Development Tools on Mac OS X systems.">Getting Started Mac OS X</a></li>
<li><a href="../cuda-getting-started-guide-for-microsoft-windows/index.html" title="This guide discusses how to install and check for correct operation of the CUDA Development Tools on Microsoft Windows systems.">Getting Started Windows</a></li>
<li><a href="../cuda-c-programming-guide/index.html" title="This guide provides a detailed discussion of the CUDA programming model and programming interface. It then describes the hardware implementation, and provides guidance on how to achieve maximum performance. The Appendixes include a list of all CUDA-enabled devices, detailed description of all extensions to the C language, listings of supported mathematical functions, C++ features supported in host and device code, details on texture fetching, technical specifications of various devices, and concludes by introducing the low-level driver API.">Programming Guide</a></li>
<li><a href="../cuda-c-best-practices-guide/index.html" title="This guide presents established parallelization and optimization techniques and explains coding metaphors and idioms that can greatly simplify programming for CUDA-capable GPU architectures. The intent is to provide guidelines for obtaining the best performance from NVIDIA GPUs using the CUDA Toolkit.">Best Practices Guide</a></li>
<li><a href="../kepler-compatibility-guide/index.html" title="This application note is intended to help developers ensure that their NVIDIA CUDA applications will run effectively on GPUs based on the NVIDIA Kepler Architecture. This document provides guidance to ensure that your software applications are compatible with Kepler.">Kepler Compatibility Guide</a></li>
<li><a href="../kepler-tuning-guide/index.html" title="Kepler is NVIDIA's next-generation architecture for CUDA compute applications. Applications that follow the best practices for the Fermi architecture should typically see speedups on the Kepler architecture without any code changes. This guide summarizes the ways that an application can be fine-tuned to gain additional speedups by leveraging Kepler architectural features.">Kepler Tuning Guide</a></li>
<li><a href="../parallel-thread-execution/index.html" title="This guide provides detailed instructions on the use of PTX, a low-level parallel thread execution virtual machine and instruction set architecture (ISA). PTX exposes the GPU as a data-parallel computing device.">PTX ISA</a></li>
<li><a href="../optimus-developer-guide/index.html" title="This document explains how CUDA APIs can be used to query for GPU capabilities in NVIDIA Optimus systems.">Developer Guide for Optimus</a></li>
<li><a href="../video-decoder/index.html" title="This document provides the video decoder API specification and the format conversion and display using DirectX or OpenGL following decode.">Video Decoder</a></li>
<li><a href="../video-encoder/index.html" title="This document provides the CUDA video encoder specifications, including the C-library API functions and encoder query parameters.">Video Encoder</a></li>
<li><a href="../inline-ptx-assembly/index.html" title="This document shows how to inline PTX (parallel thread execution) assembly language statements into CUDA code. It describes available assembler statement parameters and constraints, and the document also provides a list of some pitfalls that you may encounter.">Inline PTX Assembly</a></li>
<li><a href="../cuda-runtime-api/index.html" title="The CUDA runtime API.">CUDA Runtime API</a></li>
<li><a href="../cuda-driver-api/index.html" title="The CUDA driver API.">CUDA Driver API</a></li>
<li><a href="../cuda-math-api/index.html" title="The CUDA math API.">CUDA Math API</a></li>
<li><a href="../cublas/index.html" title="The CUBLAS library is an implementation of BLAS (Basic Linear Algebra Subprograms) on top of the NVIDIA CUDA runtime. It allows the user to access the computational resources of NVIDIA Graphical Processing Unit (GPU), but does not auto-parallelize across multiple GPUs.">CUBLAS</a></li>
<li><a href="../cufft/index.html" title="The CUFFT library user guide.">CUFFT</a></li>
<li><a href="../curand/index.html" title="The CURAND library user guide.">CURAND</a></li>
<li><a href="../cusparse/index.html" title="The CUSPARSE library user guide.">CUSPARSE</a></li>
<li><a href="../npp/index.html" title="NVIDIA NPP is a library of functions for performing CUDA accelerated processing. The initial set of functionality in the library focuses on imaging and video processing and is widely applicable for developers in these areas. NPP will evolve over time to encompass more of the compute heavy tasks in a variety of problem domains. The NPP library is written to maximize flexibility, while maintaining high performance.">NPP</a></li>
<li><a href="../thrust/index.html" title="The Thrust getting started guide.">Thrust</a></li>
<li><a href="../cuda-samples/index.html" title="This document contains a complete listing of the code samples that are included with the NVIDIA CUDA Toolkit. It describes each code sample, lists the minimum GPU specification, and provides links to the source code and white papers if available.">CUDA Samples</a></li>
<li><a href="../cuda-compiler-driver-nvcc/index.html" title="This document is a reference guide on the use of the CUDA compiler driver nvcc. Instead of being a specific CUDA compilation driver, nvcc mimics the behavior of the GNU compiler gcc, accepting a range of conventional compiler options, such as for defining macros and include/library paths, and for steering the compilation process.">NVCC</a></li>
<li><a href="../cuda-gdb/index.html" title="The NVIDIA tool for debugging CUDA applications running on Linux and Mac, providing developers with a mechanism for debugging CUDA applications running on actual hardware. CUDA-GDB is an extension to the x86-64 port of GDB, the GNU Project debugger.">CUDA-GDB</a></li>
<li><a href="../cuda-memcheck/index.html" title="CUDA-MEMCHECK is a suite of run time tools capable of precisely detecting out of bounds and misaligned memory access errors, checking device allocation leaks, reporting hardware errors and identifying shared memory data access hazards.">CUDA-MEMCHECK</a></li>
<li><a href="../nsight-eclipse-edition-getting-started-guide/index.html" title="Nsight Eclipse Edition getting started guide">Nsight Eclipse Edition</a></li>
<li><a href="../profiler-users-guide/index.html" title="This is the guide to the Profiler.">Profiler</a></li>
<li><a href="../cuda-binary-utilities/index.html" title="The application notes for cuobjdump and nvdisasm.">CUDA Binary Utilities</a></li>
<li><a href="../floating-point/index.html" title="A number of issues related to floating point accuracy and compliance are a frequent source of confusion on both CPUs and GPUs. The purpose of this white paper is to discuss the most common issues related to NVIDIA GPUs and to supplement the documentation in the CUDA C Programming Guide.">Floating Point and IEEE 754</a></li>
<li><a href="../incomplete-lu-cholesky/index.html" title="In this white paper we show how to use the CUSPARSE and CUBLAS libraries to achieve a 2x speedup over CPU in the incomplete-LU and Cholesky preconditioned iterative methods. We focus on the Bi-Conjugate Gradient Stabilized and Conjugate Gradient iterative methods, that can be used to solve large sparse nonsymmetric and symmetric positive definite linear systems, respectively. Also, we comment on the parallel sparse triangular solve, which is an essential building block in these algorithms.">Incomplete-LU and Cholesky Preconditioned Iterative Methods</a></li>
<li><a href="../libnvvm-api/index.html" title="The libNVVM API.">libNVVM API</a></li>
<li><a href="../libdevice-users-guide/index.html" title="The libdevice library is an LLVM bitcode library that implements common functions for GPU kernels.">libdevice User's Guide</a></li>
<li><a href="../nvvm-ir-spec/index.html" title="NVVM IR is a compiler IR (internal representation) based on the LLVM IR. The NVVM IR is designed to represent GPU compute kernels (for example, CUDA kernels). High-level language front-ends, like the CUDA C compiler front-end, can generate NVVM IR.">NVVM IR</a></li>
<li><a href="../cupti/index.html" title="The CUPTI API.">CUPTI</a></li>
<li><a href="../debugger-api/index.html" title="The CUDA debugger API.">Debugger API</a></li>
<li><a href="../gpudirect-rdma/index.html" title="A tool for Kepler-class GPUs and CUDA 5.0 enabling a direct path for communication between the GPU and a peer device on the PCI Express bus when the devices share the same upstream root complex using standard features of PCI Express. This document introduces the technology and describes the steps necessary to enable a RDMA for GPUDirect connection to NVIDIA GPUs within the Linux device driver model.">RDMA for GPUDirect</a></li>
</ul>
<div class="category"><span class="twiddle">▼</span><a href="index.html" title="CUDA Runtime API">CUDA Runtime API</a></div>
<ul>
<li><a href="api-sync-behavior.html#api-sync-behavior">1. API synchronization behavior </a></li>
<li><a href="modules.html#modules">2. Modules</a><ul>
<li><a href="group__CUDART__DEVICE.html#group__CUDART__DEVICE">2.1. Device Management</a></li>
<li><a href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED">2.2. Thread Management [DEPRECATED]</a></li>
<li><a href="group__CUDART__ERROR.html#group__CUDART__ERROR">2.3. Error Handling</a></li>
<li><a href="group__CUDART__STREAM.html#group__CUDART__STREAM">2.4. Stream Management</a></li>
<li><a href="group__CUDART__EVENT.html#group__CUDART__EVENT">2.5. Event Management</a></li>
<li><a href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION">2.6. Execution Control</a></li>
<li><a href="group__CUDART__MEMORY.html#group__CUDART__MEMORY">2.7. Memory Management</a></li>
<li><a href="group__CUDART__UNIFIED.html#group__CUDART__UNIFIED">2.8. Unified Addressing</a></li>
<li><a href="group__CUDART__PEER.html#group__CUDART__PEER">2.9. Peer Device Memory Access</a></li>
<li><a href="group__CUDART__OPENGL.html#group__CUDART__OPENGL">2.10. OpenGL Interoperability</a></li>
<li><a href="group__CUDART__OPENGL__DEPRECATED.html#group__CUDART__OPENGL__DEPRECATED">2.11. OpenGL Interoperability [DEPRECATED]</a></li>
<li><a href="group__CUDART__D3D9.html#group__CUDART__D3D9">2.12. Direct3D 9 Interoperability</a></li>
<li><a href="group__CUDART__D3D9__DEPRECATED.html#group__CUDART__D3D9__DEPRECATED">2.13. Direct3D 9 Interoperability [DEPRECATED]</a></li>
<li><a href="group__CUDART__D3D10.html#group__CUDART__D3D10">2.14. Direct3D 10 Interoperability</a></li>
<li><a href="group__CUDART__D3D10__DEPRECATED.html#group__CUDART__D3D10__DEPRECATED">2.15. Direct3D 10 Interoperability [DEPRECATED]</a></li>
<li><a href="group__CUDART__D3D11.html#group__CUDART__D3D11">2.16. Direct3D 11 Interoperability</a></li>
<li><a href="group__CUDART__D3D11__DEPRECATED.html#group__CUDART__D3D11__DEPRECATED">2.17. Direct3D 11 Interoperability [DEPRECATED]</a></li>
<li><a href="group__CUDART__VDPAU.html#group__CUDART__VDPAU">2.18. VDPAU Interoperability</a></li>
<li><a href="group__CUDART__INTEROP.html#group__CUDART__INTEROP">2.19. Graphics Interoperability</a></li>
<li><a href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE">2.20. Texture Reference Management</a></li>
<li><a href="group__CUDART__SURFACE.html#group__CUDART__SURFACE">2.21. Surface Reference Management</a></li>
<li><a href="group__CUDART__TEXTURE__OBJECT.html#group__CUDART__TEXTURE__OBJECT">2.22. Texture Object Management</a></li>
<li><a href="group__CUDART__SURFACE__OBJECT.html#group__CUDART__SURFACE__OBJECT">2.23. Surface Object Management</a></li>
<li><a href="group__CUDART____VERSION.html#group__CUDART____VERSION">2.24. Version Management</a></li>
<li><a href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL">2.25. C++ API Routines</a></li>
<li><a href="group__CUDART__DRIVER.html#group__CUDART__DRIVER">2.26. Interactions with the CUDA Driver API</a></li>
<li><a href="group__CUDART__PROFILER.html#group__CUDART__PROFILER">2.27. Profiler Control</a></li>
<li><a href="group__CUDART__TYPES.html#group__CUDART__TYPES">2.28. Data types used by CUDA Runtime</a></li>
</ul>
</li>
<li><a href="annotated.html#annotated">3. Data Structures</a><ul>
<li><a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc">3.1. cudaChannelFormatDesc</a></li>
<li><a href="structcudaDeviceProp.html#structcudaDeviceProp">3.2. cudaDeviceProp</a></li>
<li><a href="structcudaExtent.html#structcudaExtent">3.3. cudaExtent</a></li>
<li><a href="structcudaFuncAttributes.html#structcudaFuncAttributes">3.4. cudaFuncAttributes</a></li>
<li><a href="structcudaIpcEventHandle__t.html#structcudaIpcEventHandle__t">3.5. cudaIpcEventHandle_t</a></li>
<li><a href="structcudaIpcMemHandle__t.html#structcudaIpcMemHandle__t">3.6. cudaIpcMemHandle_t</a></li>
<li><a href="structcudaMemcpy3DParms.html#structcudaMemcpy3DParms">3.7. cudaMemcpy3DParms</a></li>
<li><a href="structcudaMemcpy3DPeerParms.html#structcudaMemcpy3DPeerParms">3.8. cudaMemcpy3DPeerParms</a></li>
<li><a href="structcudaPitchedPtr.html#structcudaPitchedPtr">3.9. cudaPitchedPtr</a></li>
<li><a href="structcudaPointerAttributes.html#structcudaPointerAttributes">3.10. cudaPointerAttributes</a></li>
<li><a href="structcudaPos.html#structcudaPos">3.11. cudaPos</a></li>
<li><a href="structcudaResourceDesc.html#structcudaResourceDesc">3.12. cudaResourceDesc</a></li>
<li><a href="structcudaResourceViewDesc.html#structcudaResourceViewDesc">3.13. cudaResourceViewDesc</a></li>
<li><a href="structcudaTextureDesc.html#structcudaTextureDesc">3.14. cudaTextureDesc</a></li>
<li><a href="structsurfaceReference.html#structsurfaceReference">3.15. surfaceReference</a></li>
<li><a href="structtextureReference.html#structtextureReference">3.16. textureReference</a></li>
</ul>
</li>
<li><a href="functions.html#functions">4. Data Fields</a></li>
<li><a href="deprecated.html#deprecated">5. Deprecated List</a></li>
<li><a href="notices-header.html#notices-header">Notices</a><ul></ul>
</li>
</ul>
</nav>
<nav id="search-results">
<h2>Search Results</h2>
<ol></ol>
</nav>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/formatting/common.min.js"></script>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/scripts/omniture/s_code_us_dev_aut1-nolinktrackin.js"></script>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/scripts/omniture/omniture.js"></script>
<noscript><a href="http://www.omniture.com" title="Web Analytics"><img src="http://omniture.nvidia.com/b/ss/nvidiacudadocs/1/H.17--NS/0" height="1" width="1" border="0" alt=""></img></a></noscript>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/scripts/google-analytics/google-analytics-write.js"></script>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/scripts/google-analytics/google-analytics-tracker.js"></script>
</body>
</html>
