<!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="Data types used by CUDA Runtime"></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__TYPES"></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/scripts/tynt/tynt.js"></script>
<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>
<script type="text/javascript" charset="utf-8" src="../common/formatting/jquery.scrollintoview.min.js"></script>
<script type="text/javascript" src="../search/htmlFileList.js"></script>
<script type="text/javascript" src="../search/htmlFileInfoList.js"></script>
<script type="text/javascript" src="../search/nwSearchFnt.min.js"></script>
<script type="text/javascript" src="../search/stemmers/en_stemmer.min.js"></script>
<script type="text/javascript" src="../search/index-1.js"></script>
<script type="text/javascript" src="../search/index-2.js"></script>
<script type="text/javascript" src="../search/index-3.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>
<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>
<div id="site-content">
<nav id="site-nav">
<div class="category closed"><a href="../index.html" title="The root of the site.">CUDA Toolkit
v6.5</a></div>
<div class="category"><a href="index.html" title="CUDA Runtime API">CUDA Runtime API</a></div>
<ul>
<li>
<div class="section-link"><a href="api-sync-behavior.html#api-sync-behavior">1. API synchronization behavior </a></div>
</li>
<li>
<div class="section-link"><a href="stream-sync-behavior.html#stream-sync-behavior">2. Stream synchronization behavior</a></div>
</li>
<li>
<div class="section-link"><a href="modules.html#modules">3. Modules</a></div>
<ul>
<li>
<div class="section-link"><a href="group__CUDART__DEVICE.html#group__CUDART__DEVICE">3.1. Device Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED">3.2. Thread Management [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__ERROR.html#group__CUDART__ERROR">3.3. Error Handling</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__STREAM.html#group__CUDART__STREAM">3.4. Stream Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__EVENT.html#group__CUDART__EVENT">3.5. Event Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION">3.6. Execution Control</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__OCCUPANCY.html#group__CUDART__OCCUPANCY">3.7. Occupancy</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__MEMORY.html#group__CUDART__MEMORY">3.8. Memory Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__UNIFIED.html#group__CUDART__UNIFIED">3.9. Unified Addressing</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__PEER.html#group__CUDART__PEER">3.10. Peer Device Memory Access</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__OPENGL.html#group__CUDART__OPENGL">3.11. OpenGL Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__OPENGL__DEPRECATED.html#group__CUDART__OPENGL__DEPRECATED">3.12. OpenGL Interoperability [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D9.html#group__CUDART__D3D9">3.13. Direct3D 9 Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D9__DEPRECATED.html#group__CUDART__D3D9__DEPRECATED">3.14. Direct3D 9 Interoperability [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D10.html#group__CUDART__D3D10">3.15. Direct3D 10 Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D10__DEPRECATED.html#group__CUDART__D3D10__DEPRECATED">3.16. Direct3D 10 Interoperability [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D11.html#group__CUDART__D3D11">3.17. Direct3D 11 Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D11__DEPRECATED.html#group__CUDART__D3D11__DEPRECATED">3.18. Direct3D 11 Interoperability [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__VDPAU.html#group__CUDART__VDPAU">3.19. VDPAU Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__INTEROP.html#group__CUDART__INTEROP">3.20. Graphics Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE">3.21. Texture Reference Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__SURFACE.html#group__CUDART__SURFACE">3.22. Surface Reference Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__TEXTURE__OBJECT.html#group__CUDART__TEXTURE__OBJECT">3.23. Texture Object Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__SURFACE__OBJECT.html#group__CUDART__SURFACE__OBJECT">3.24. Surface Object Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART____VERSION.html#group__CUDART____VERSION">3.25. Version Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL">3.26. C++ API Routines</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__DRIVER.html#group__CUDART__DRIVER">3.27. Interactions with the CUDA Driver API</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__PROFILER.html#group__CUDART__PROFILER">3.28. Profiler Control</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES">3.29. Data types used by CUDA Runtime</a></div>
</li>
</ul>
</li>
<li>
<div class="section-link"><a href="annotated.html#annotated">4. Data Structures</a></div>
<ul>
<li>
<div class="section-link"><a href="class____cudaOccupancyB2DHelper.html#class____cudaOccupancyB2DHelper">4.1. __cudaOccupancyB2DHelper</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc">4.2. cudaChannelFormatDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaDeviceProp.html#structcudaDeviceProp">4.3. cudaDeviceProp</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaExtent.html#structcudaExtent">4.4. cudaExtent</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaFuncAttributes.html#structcudaFuncAttributes">4.5. cudaFuncAttributes</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaIpcEventHandle__t.html#structcudaIpcEventHandle__t">4.6. cudaIpcEventHandle_t</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaIpcMemHandle__t.html#structcudaIpcMemHandle__t">4.7. cudaIpcMemHandle_t</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaMemcpy3DParms.html#structcudaMemcpy3DParms">4.8. cudaMemcpy3DParms</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaMemcpy3DPeerParms.html#structcudaMemcpy3DPeerParms">4.9. cudaMemcpy3DPeerParms</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaPitchedPtr.html#structcudaPitchedPtr">4.10. cudaPitchedPtr</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaPointerAttributes.html#structcudaPointerAttributes">4.11. cudaPointerAttributes</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaPos.html#structcudaPos">4.12. cudaPos</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaResourceDesc.html#structcudaResourceDesc">4.13. cudaResourceDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaResourceViewDesc.html#structcudaResourceViewDesc">4.14. cudaResourceViewDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaTextureDesc.html#structcudaTextureDesc">4.15. cudaTextureDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structsurfaceReference.html#structsurfaceReference">4.16. surfaceReference</a></div>
</li>
<li>
<div class="section-link"><a href="structtextureReference.html#structtextureReference">4.17. textureReference</a></div>
</li>
</ul>
</li>
<li>
<div class="section-link"><a href="functions.html#functions">5. Data Fields</a></div>
</li>
<li>
<div class="section-link"><a href="deprecated.html#deprecated">6. Deprecated List</a></div>
</li>
<li>
<div class="section-link"><a href="notices-header.html#notices-header">Notices</a></div>
<ul></ul>
</li>
</ul>
</nav>
<div id="resize-nav"></div>
<nav id="search-results">
<h2>Search Results</h2>
<ol></ol>
</nav>
<div id="contents-container">
<div id="breadcrumbs-container">
<div id="breadcrumbs"><a href="group__CUDART__PROFILER.html" shape="rect">< Previous</a> | <a href="annotated.html" shape="rect">Next ></a></div>
<div id="release-info">CUDA Runtime API
(<a href="../../pdf/CUDA_Runtime_API.pdf">PDF</a>)
-
v6.5
(<a href="https://developer.nvidia.com/cuda-toolkit-archive">older</a>)
-
Last updated August 1, 2014
-
<a href="mailto:cudatools@nvidia.com?subject=CUDA Toolkit Documentation Feedback: CUDA Runtime API">Send Feedback</a>
-
<span class="st_facebook"></span><span class="st_twitter"></span><span class="st_linkedin"></span><span class="st_reddit"></span><span class="st_slashdot"></span><span class="st_tumblr"></span><span class="st_sharethis"></span></div>
</div>
<article id="contents">
<div class="topic reference apiRef apiPackage cppModule" id="group__CUDART__TYPES"><a name="group__CUDART__TYPES" shape="rect">
<!-- --></a><h2 class="topictitle2 cppModule">3.29. Data types used by CUDA Runtime</h2>
<div class="section">
<p></p>
</div>
<h3 class="fake_sectiontitle member_header">Classes</h3>
<dl class="members">
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" shape="rect">cudaChannelFormatDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaDeviceProp.html#structcudaDeviceProp" shape="rect">cudaDeviceProp</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaDeviceProp.html#structcudaDeviceProp" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaExtent.html#structcudaExtent" shape="rect">cudaExtent</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaExtent.html#structcudaExtent" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaFuncAttributes.html#structcudaFuncAttributes" shape="rect">cudaFuncAttributes</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaFuncAttributes.html#structcudaFuncAttributes" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaIpcEventHandle__t.html#structcudaIpcEventHandle__t" shape="rect">cudaIpcEventHandle_t</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaIpcEventHandle__t.html#structcudaIpcEventHandle__t" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaIpcMemHandle__t.html#structcudaIpcMemHandle__t" shape="rect">cudaIpcMemHandle_t</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaIpcMemHandle__t.html#structcudaIpcMemHandle__t" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaMemcpy3DParms.html#structcudaMemcpy3DParms" shape="rect">cudaMemcpy3DParms</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaMemcpy3DParms.html#structcudaMemcpy3DParms" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaMemcpy3DPeerParms.html#structcudaMemcpy3DPeerParms" shape="rect">cudaMemcpy3DPeerParms</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaMemcpy3DPeerParms.html#structcudaMemcpy3DPeerParms" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaPitchedPtr.html#structcudaPitchedPtr" shape="rect">cudaPitchedPtr</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaPitchedPtr.html#structcudaPitchedPtr" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaPointerAttributes.html#structcudaPointerAttributes" shape="rect">cudaPointerAttributes</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaPointerAttributes.html#structcudaPointerAttributes" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaPos.html#structcudaPos" shape="rect">cudaPos</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaPos.html#structcudaPos" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaResourceDesc.html#structcudaResourceDesc" shape="rect">cudaResourceDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaResourceDesc.html#structcudaResourceDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaResourceViewDesc.html#structcudaResourceViewDesc" shape="rect">cudaResourceViewDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaResourceViewDesc.html#structcudaResourceViewDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaTextureDesc.html#structcudaTextureDesc" shape="rect">cudaTextureDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaTextureDesc.html#structcudaTextureDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structsurfaceReference.html#structsurfaceReference" shape="rect">surfaceReference</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structsurfaceReference.html#structsurfaceReference" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structtextureReference.html#structtextureReference" shape="rect">textureReference</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structtextureReference.html#structtextureReference" class="link" title="" shape="rect"></a></dd>
</dl>
<h3 class="fake_sectiontitle member_header">Defines</h3>
<dl class="members">
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g38818d647e61a5d15fb8012fe54c2d24" shape="rect">CUDA_IPC_HANDLE_SIZE</a> 64</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g802843d69ca8be35ee050ff66782179e" shape="rect">cudaArrayCubemap</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6c47e87081bfd4f6030937f99ef12412" shape="rect">cudaArrayDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6d9a27dfb1207df13de0e822f75f4ab8" shape="rect">cudaArrayLayered</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g8cb5bdac32ad53c423992a125b3f9a66" shape="rect">cudaArraySurfaceLoadStore</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g142b19a14d56a03b1e410430aa5202d1" shape="rect">cudaArrayTextureGather</a> 0x08</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g130ddae663f1873258fee5a6e0808b71" shape="rect">cudaDeviceBlockingSync</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gda5f97298bf704dd3b04cbac4819e6e3" shape="rect">cudaDeviceLmemResizeToMax</a> 0x10</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g3762be9cccdd809a4ca128354fd134b0" shape="rect">cudaDeviceMapHost</a> 0x08</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gc50dd5d226be88b768de22e849c9bf7a" shape="rect">cudaDeviceMask</a> 0x1f</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g1f938b9d13391758b22f0d0d2faa3e47" shape="rect">cudaDevicePropDontCare</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g3ade1dbaf4b222b22733cdfdcc026075" shape="rect">cudaDeviceScheduleAuto</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" shape="rect">cudaDeviceScheduleBlockingSync</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g008de63abd7ba8da0f5f13ef7317fd29" shape="rect">cudaDeviceScheduleMask</a> 0x07</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gf01347c3dafebf07e1a0b4321a030a63" shape="rect">cudaDeviceScheduleSpin</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gbc13c52d342c67ebf0f1f7af937735a8" shape="rect">cudaDeviceScheduleYield</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g26509a522be9d449aa7c8c279612452d" shape="rect">cudaEventBlockingSync</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6f8811acffcc133b5e4a50de6646d18e" shape="rect">cudaEventDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1ga5d3eff7c3623e2be533968d9cc1ee7e" shape="rect">cudaEventDisableTiming</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g49ec9cd742f8a3f6fde4ee72a66326f6" shape="rect">cudaEventInterprocess</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g1e00f7734325eb38d75f3ffeae6acac8" shape="rect">cudaHostAllocDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" shape="rect">cudaHostAllocMapped</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gc46ce76be41cf79774331cc8cfceb52b" shape="rect">cudaHostAllocPortable</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g3a7db37d02ce0b2350067ab639ef321c" shape="rect">cudaHostAllocWriteCombined</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g91ca01bef4ecb16ca98b8e129ff6427f" shape="rect">cudaHostRegisterDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g838b73458521c60f502efd19db0e365d" shape="rect">cudaHostRegisterMapped</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g36977255e5c778f7e4362d32d6b1cecd" shape="rect">cudaHostRegisterPortable</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g60f28a5142ee7ae0336dfa83fd54e006" shape="rect">cudaIpcMemLazyEnablePeerAccess</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">cudaMemAttachHost</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">cudaMemAttachSingle</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g666bfab4a42e799d74bc07269f9bcd9b" shape="rect">cudaPeerAccessDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1ged347a89ec289c787faa116b851708fc" shape="rect">cudaStreamDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g5dbd11a1723d9f5938a133cedbc525e3" shape="rect">cudaStreamNonBlocking</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
</dl>
<h3 class="fake_sectiontitle member_header">Typedefs</h3>
<dl class="members">
<dt><span class="member_type">typedef cudaArray * </span><span class="member_name"><a href="#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" shape="rect">cudaArray_const_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef cudaArray * </span><span class="member_name"><a href="#group__CUDART__TYPES_1gaf8b3ba752727d996074a71ee997ce68" shape="rect">cudaArray_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" title="" shape="rect">enumcudaError</a> </span><span class="member_name"><a href="#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" shape="rect">cudaError_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef CUevent_st * </span><span class="member_name"><a href="#group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" shape="rect">cudaEvent_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef cudaGraphicsResource * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1gf58dd8d3c7a65714ff7f5459adbf7e6f" shape="rect">cudaGraphicsResource_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef cudaMipmappedArray * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" shape="rect">cudaMipmappedArray_const_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef cudaMipmappedArray * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1g1b03ad14fc0ab86f8b033837f5562d8a" shape="rect">cudaMipmappedArray_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" title="" shape="rect">enumcudaOutputMode</a> </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1ge1e4fa3423d204e9f927703561c36c8f" shape="rect">cudaOutputMode_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef CUstream_st * </span><span class="member_name"><a href="#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" shape="rect">cudaStream_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef unsigned long long </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1gbe57cf2ccbe7f9d696f18808dd634c0a" shape="rect">cudaSurfaceObject_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef unsigned long long </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1g83eb271ebc4cb2817e66d7c752f0c29b" shape="rect">cudaTextureObject_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef CUuuid_st </span><span class="member_name"><a href="#group__CUDART__TYPES_1gbc782b3ec2c70c11b945629e1e0542b9" shape="rect">cudaUUID_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
</dl>
<h3 class="fake_sectiontitle member_header">Enumerations</h3>
<dl class="members">
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" shape="rect">cudaChannelFormatKind</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g7eb25f5413a962faad0956d92bae10d0" shape="rect">cudaComputeMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g49e2f8c2c0bd6fe264f2fc970912e5cd" shape="rect">cudaDeviceAttr</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" shape="rect">cudaError</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" shape="rect">cudaFuncCache</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gbf3ce16a621826a09263b8a58902fee8" shape="rect">cudaGraphicsCubeFace</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g2c3c3a69caaf333d29d0b38b75de5ffd" shape="rect">cudaGraphicsMapFlags</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gd17cc29b28205bbe32ac575eba16c277" shape="rect">cudaGraphicsRegisterFlags</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" shape="rect">cudaLimit</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" shape="rect">cudaMemcpyKind</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g13de56a8fe75569530ecc3a3106e9b6d" shape="rect">cudaMemoryType</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" shape="rect">cudaOutputMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g067b774c0e639817a00a972c8e2c203c" shape="rect">cudaResourceType</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6b3a50368a0aa592f65e928adca9b929" shape="rect">cudaResourceViewFormat</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6e62d15f3c224625e8c9aa946f1709a6" shape="rect">cudaSharedMemConfig</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gdc002e3c2a4fd592efa944e2c73a10fb" shape="rect">cudaSurfaceBoundaryMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g427be57cb8aa90479139bba92267150f" shape="rect">cudaSurfaceFormatMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g03e1bbd2c491d809279c7a47e2cd0351" shape="rect">cudaTextureAddressMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gee4adb3d1b062cf05374de09325a82d5" shape="rect">cudaTextureFilterMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gd9266d02be93809558036ec4f3d5f43d" shape="rect">cudaTextureReadMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
</dl>
<div class="description">
<h3 class="sectiontitle">Defines</h3>
<dl class="description">
<dt class="description"><a name="group__CUDART__TYPES_1g38818d647e61a5d15fb8012fe54c2d24" id="group__CUDART__TYPES_1g38818d647e61a5d15fb8012fe54c2d24" shape="rect">
<!-- --></a><span>#define CUDA_IPC_HANDLE_SIZE 64</span></dt>
<dd class="description">
<div class="section">
<p>CUDA IPC Handle Size </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g802843d69ca8be35ee050ff66782179e" id="group__CUDART__TYPES_1g802843d69ca8be35ee050ff66782179e" shape="rect">
<!-- --></a><span>#define cudaArrayCubemap 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaMalloc3DArray to create a cubemap CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6c47e87081bfd4f6030937f99ef12412" id="group__CUDART__TYPES_1g6c47e87081bfd4f6030937f99ef12412" shape="rect">
<!-- --></a><span>#define cudaArrayDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default CUDA array allocation flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6d9a27dfb1207df13de0e822f75f4ab8" id="group__CUDART__TYPES_1g6d9a27dfb1207df13de0e822f75f4ab8" shape="rect">
<!-- --></a><span>#define cudaArrayLayered 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaMalloc3DArray to create a layered CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g8cb5bdac32ad53c423992a125b3f9a66" id="group__CUDART__TYPES_1g8cb5bdac32ad53c423992a125b3f9a66" shape="rect">
<!-- --></a><span>#define cudaArraySurfaceLoadStore 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaMallocArray or cudaMalloc3DArray in order to bind surfaces to the CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g142b19a14d56a03b1e410430aa5202d1" id="group__CUDART__TYPES_1g142b19a14d56a03b1e410430aa5202d1" shape="rect">
<!-- --></a><span>#define cudaArrayTextureGather 0x08</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaMallocArray or cudaMalloc3DArray in order to perform texture gather operations on the CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g130ddae663f1873258fee5a6e0808b71" id="group__CUDART__TYPES_1g130ddae663f1873258fee5a6e0808b71" shape="rect">
<!-- --></a><span>#define cudaDeviceBlockingSync 0x04</span></dt>
<dd class="description">
<div class="section">
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000039" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This flag was deprecated as of CUDA 4.0 and replaced with <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" shape="rect">cudaDeviceScheduleBlockingSync</a>. </span></p>
<p>Device flag - Use blocking synchronization </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gda5f97298bf704dd3b04cbac4819e6e3" id="group__CUDART__TYPES_1gda5f97298bf704dd3b04cbac4819e6e3" shape="rect">
<!-- --></a><span>#define cudaDeviceLmemResizeToMax 0x10</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Keep local memory allocation after launch </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g3762be9cccdd809a4ca128354fd134b0" id="group__CUDART__TYPES_1g3762be9cccdd809a4ca128354fd134b0" shape="rect">
<!-- --></a><span>#define cudaDeviceMapHost 0x08</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Support mapped pinned allocations </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gc50dd5d226be88b768de22e849c9bf7a" id="group__CUDART__TYPES_1gc50dd5d226be88b768de22e849c9bf7a" shape="rect">
<!-- --></a><span>#define cudaDeviceMask 0x1f</span></dt>
<dd class="description">
<div class="section">
<p>Device flags mask </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g1f938b9d13391758b22f0d0d2faa3e47" id="group__CUDART__TYPES_1g1f938b9d13391758b22f0d0d2faa3e47" shape="rect">
<!-- --></a><span>#define cudaDevicePropDontCare </span></dt>
<dd class="description">
<div class="section">
<p>Empty device properties </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g3ade1dbaf4b222b22733cdfdcc026075" id="group__CUDART__TYPES_1g3ade1dbaf4b222b22733cdfdcc026075" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleAuto 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Automatic scheduling </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" id="group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleBlockingSync 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Use blocking synchronization </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g008de63abd7ba8da0f5f13ef7317fd29" id="group__CUDART__TYPES_1g008de63abd7ba8da0f5f13ef7317fd29" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleMask 0x07</span></dt>
<dd class="description">
<div class="section">
<p>Device schedule flags mask </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gf01347c3dafebf07e1a0b4321a030a63" id="group__CUDART__TYPES_1gf01347c3dafebf07e1a0b4321a030a63" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleSpin 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Spin default scheduling </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbc13c52d342c67ebf0f1f7af937735a8" id="group__CUDART__TYPES_1gbc13c52d342c67ebf0f1f7af937735a8" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleYield 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Yield default scheduling </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g26509a522be9d449aa7c8c279612452d" id="group__CUDART__TYPES_1g26509a522be9d449aa7c8c279612452d" shape="rect">
<!-- --></a><span>#define cudaEventBlockingSync 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Event uses blocking synchronization </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6f8811acffcc133b5e4a50de6646d18e" id="group__CUDART__TYPES_1g6f8811acffcc133b5e4a50de6646d18e" shape="rect">
<!-- --></a><span>#define cudaEventDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default event flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1ga5d3eff7c3623e2be533968d9cc1ee7e" id="group__CUDART__TYPES_1ga5d3eff7c3623e2be533968d9cc1ee7e" shape="rect">
<!-- --></a><span>#define cudaEventDisableTiming 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Event will not record timing data </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g49ec9cd742f8a3f6fde4ee72a66326f6" id="group__CUDART__TYPES_1g49ec9cd742f8a3f6fde4ee72a66326f6" shape="rect">
<!-- --></a><span>#define cudaEventInterprocess 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Event is suitable for interprocess use. cudaEventDisableTiming must be set </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g1e00f7734325eb38d75f3ffeae6acac8" id="group__CUDART__TYPES_1g1e00f7734325eb38d75f3ffeae6acac8" shape="rect">
<!-- --></a><span>#define cudaHostAllocDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default page-locked allocation flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" id="group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" shape="rect">
<!-- --></a><span>#define cudaHostAllocMapped 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Map allocation into device space </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gc46ce76be41cf79774331cc8cfceb52b" id="group__CUDART__TYPES_1gc46ce76be41cf79774331cc8cfceb52b" shape="rect">
<!-- --></a><span>#define cudaHostAllocPortable 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Pinned memory accessible by all CUDA contexts </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g3a7db37d02ce0b2350067ab639ef321c" id="group__CUDART__TYPES_1g3a7db37d02ce0b2350067ab639ef321c" shape="rect">
<!-- --></a><span>#define cudaHostAllocWriteCombined 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Write-combined memory </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g91ca01bef4ecb16ca98b8e129ff6427f" id="group__CUDART__TYPES_1g91ca01bef4ecb16ca98b8e129ff6427f" shape="rect">
<!-- --></a><span>#define cudaHostRegisterDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default host memory registration flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g838b73458521c60f502efd19db0e365d" id="group__CUDART__TYPES_1g838b73458521c60f502efd19db0e365d" shape="rect">
<!-- --></a><span>#define cudaHostRegisterMapped 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Map registered memory into device space </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g36977255e5c778f7e4362d32d6b1cecd" id="group__CUDART__TYPES_1g36977255e5c778f7e4362d32d6b1cecd" shape="rect">
<!-- --></a><span>#define cudaHostRegisterPortable 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Pinned memory accessible by all CUDA contexts </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g60f28a5142ee7ae0336dfa83fd54e006" id="group__CUDART__TYPES_1g60f28a5142ee7ae0336dfa83fd54e006" shape="rect">
<!-- --></a><span>#define cudaIpcMemLazyEnablePeerAccess 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Automatically enable peer access between remote devices as needed </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" id="group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">
<!-- --></a><span>#define cudaMemAttachGlobal 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Memory can be accessed by any stream on any device </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" id="group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">
<!-- --></a><span>#define cudaMemAttachHost 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Memory cannot be accessed by any stream on any device </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" id="group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">
<!-- --></a><span>#define cudaMemAttachSingle 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Memory can only be accessed by a single stream on the associated device </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g666bfab4a42e799d74bc07269f9bcd9b" id="group__CUDART__TYPES_1g666bfab4a42e799d74bc07269f9bcd9b" shape="rect">
<!-- --></a><span>#define cudaPeerAccessDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default peer addressing enable flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1ged347a89ec289c787faa116b851708fc" id="group__CUDART__TYPES_1ged347a89ec289c787faa116b851708fc" shape="rect">
<!-- --></a><span>#define cudaStreamDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default stream flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g5dbd11a1723d9f5938a133cedbc525e3" id="group__CUDART__TYPES_1g5dbd11a1723d9f5938a133cedbc525e3" shape="rect">
<!-- --></a><span>#define cudaStreamNonBlocking 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Stream does not synchronize with stream 0 (the NULL stream) </p>
</div>
</dd>
</dl>
</div>
<div class="description">
<h3 class="sectiontitle">Typedefs</h3>
<dl class="description">
<dt class="description"><a name="group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" id="group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" shape="rect">
<!-- --></a><span>typedef cudaArray * cudaArray_const_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA array (as source copy argument) </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gaf8b3ba752727d996074a71ee997ce68" id="group__CUDART__TYPES_1gaf8b3ba752727d996074a71ee997ce68" shape="rect">
<!-- --></a><span>typedef cudaArray * cudaArray_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" id="group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" shape="rect">
<!-- --></a><span>typedef <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" title="" shape="rect">enumcudaError</a> cudaError_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA Error types </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" id="group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" shape="rect">
<!-- --></a><span>typedef CUevent_st * cudaEvent_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA event types </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gf58dd8d3c7a65714ff7f5459adbf7e6f" id="group__CUDART__TYPES_1gf58dd8d3c7a65714ff7f5459adbf7e6f" shape="rect">
<!-- --></a><span>typedef cudaGraphicsResource * cudaGraphicsResource_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA graphics resource types </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" id="group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" shape="rect">
<!-- --></a><span>typedef cudaMipmappedArray * cudaMipmappedArray_const_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA mipmapped array (as source argument) </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g1b03ad14fc0ab86f8b033837f5562d8a" id="group__CUDART__TYPES_1g1b03ad14fc0ab86f8b033837f5562d8a" shape="rect">
<!-- --></a><span>typedef cudaMipmappedArray * cudaMipmappedArray_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA mipmapped array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1ge1e4fa3423d204e9f927703561c36c8f" id="group__CUDART__TYPES_1ge1e4fa3423d204e9f927703561c36c8f" shape="rect">
<!-- --></a><span>typedef <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" title="" shape="rect">enumcudaOutputMode</a> cudaOutputMode_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA output file modes </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" id="group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" shape="rect">
<!-- --></a><span>typedef CUstream_st * cudaStream_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA stream </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbe57cf2ccbe7f9d696f18808dd634c0a" id="group__CUDART__TYPES_1gbe57cf2ccbe7f9d696f18808dd634c0a" shape="rect">
<!-- --></a><span>typedef unsigned long long cudaSurfaceObject_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA Surface object </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g83eb271ebc4cb2817e66d7c752f0c29b" id="group__CUDART__TYPES_1g83eb271ebc4cb2817e66d7c752f0c29b" shape="rect">
<!-- --></a><span>typedef unsigned long long cudaTextureObject_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA texture object </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbc782b3ec2c70c11b945629e1e0542b9" id="group__CUDART__TYPES_1gbc782b3ec2c70c11b945629e1e0542b9" shape="rect">
<!-- --></a><span>typedef CUuuid_st cudaUUID_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA UUID types </p>
</div>
</dd>
</dl>
</div>
<div class="description">
<h3 class="sectiontitle">Enumerations</h3>
<dl class="description">
<dt class="description"><a name="group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" id="group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" shape="rect">
<!-- --></a><span>enum cudaChannelFormatKind</span></dt>
<dd class="description">
<div class="section">
<p>Channel format kind </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaChannelFormatKindSigned = <span class="ph ph apiData">0</span></span></dt>
<dd>Signed channel format </dd>
<dt><span class="enum-member-name-def">cudaChannelFormatKindUnsigned = <span class="ph ph apiData">1</span></span></dt>
<dd>Unsigned channel format </dd>
<dt><span class="enum-member-name-def">cudaChannelFormatKindFloat = <span class="ph ph apiData">2</span></span></dt>
<dd>Float channel format </dd>
<dt><span class="enum-member-name-def">cudaChannelFormatKindNone = <span class="ph ph apiData">3</span></span></dt>
<dd>No channel format </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g7eb25f5413a962faad0956d92bae10d0" id="group__CUDART__TYPES_1g7eb25f5413a962faad0956d92bae10d0" shape="rect">
<!-- --></a><span>enum cudaComputeMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA device compute modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaComputeModeDefault = <span class="ph ph apiData">0</span></span></dt>
<dd>Default compute mode (Multiple threads can use <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g418c299b069c4803bfb7cab4943da383" title="Set device to be used for GPU executions." shape="rect">cudaSetDevice()</a> with this device)
</dd>
<dt><span class="enum-member-name-def">cudaComputeModeExclusive = <span class="ph ph apiData">1</span></span></dt>
<dd>Compute-exclusive-thread mode (Only one thread in one process will be able to use <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g418c299b069c4803bfb7cab4943da383" title="Set device to be used for GPU executions." shape="rect">cudaSetDevice()</a> with this device)
</dd>
<dt><span class="enum-member-name-def">cudaComputeModeProhibited = <span class="ph ph apiData">2</span></span></dt>
<dd>Compute-prohibited mode (No threads can use <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g418c299b069c4803bfb7cab4943da383" title="Set device to be used for GPU executions." shape="rect">cudaSetDevice()</a> with this device)
</dd>
<dt><span class="enum-member-name-def">cudaComputeModeExclusiveProcess = <span class="ph ph apiData">3</span></span></dt>
<dd>Compute-exclusive-process mode (Many threads in one process will be able to use <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g418c299b069c4803bfb7cab4943da383" title="Set device to be used for GPU executions." shape="rect">cudaSetDevice()</a> with this device)
</dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g49e2f8c2c0bd6fe264f2fc970912e5cd" id="group__CUDART__TYPES_1g49e2f8c2c0bd6fe264f2fc970912e5cd" shape="rect">
<!-- --></a><span>enum cudaDeviceAttr</span></dt>
<dd class="description">
<div class="section">
<p>CUDA device attributes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaDevAttrMaxThreadsPerBlock = <span class="ph ph apiData">1</span></span></dt>
<dd>Maximum number of threads per block </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxBlockDimX = <span class="ph ph apiData">2</span></span></dt>
<dd>Maximum block dimension X </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxBlockDimY = <span class="ph ph apiData">3</span></span></dt>
<dd>Maximum block dimension Y </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxBlockDimZ = <span class="ph ph apiData">4</span></span></dt>
<dd>Maximum block dimension Z </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxGridDimX = <span class="ph ph apiData">5</span></span></dt>
<dd>Maximum grid dimension X </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxGridDimY = <span class="ph ph apiData">6</span></span></dt>
<dd>Maximum grid dimension Y </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxGridDimZ = <span class="ph ph apiData">7</span></span></dt>
<dd>Maximum grid dimension Z </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSharedMemoryPerBlock = <span class="ph ph apiData">8</span></span></dt>
<dd>Maximum shared memory available per block in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrTotalConstantMemory = <span class="ph ph apiData">9</span></span></dt>
<dd>Memory available on device for __constant__ variables in a CUDA C kernel in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrWarpSize = <span class="ph ph apiData">10</span></span></dt>
<dd>Warp size in threads </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxPitch = <span class="ph ph apiData">11</span></span></dt>
<dd>Maximum pitch in bytes allowed by memory copies </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxRegistersPerBlock = <span class="ph ph apiData">12</span></span></dt>
<dd>Maximum number of 32-bit registers available per block </dd>
<dt><span class="enum-member-name-def">cudaDevAttrClockRate = <span class="ph ph apiData">13</span></span></dt>
<dd>Peak clock frequency in kilohertz </dd>
<dt><span class="enum-member-name-def">cudaDevAttrTextureAlignment = <span class="ph ph apiData">14</span></span></dt>
<dd>Alignment requirement for textures </dd>
<dt><span class="enum-member-name-def">cudaDevAttrGpuOverlap = <span class="ph ph apiData">15</span></span></dt>
<dd>Device can possibly copy memory and execute a kernel concurrently </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMultiProcessorCount = <span class="ph ph apiData">16</span></span></dt>
<dd>Number of multiprocessors on device </dd>
<dt><span class="enum-member-name-def">cudaDevAttrKernelExecTimeout = <span class="ph ph apiData">17</span></span></dt>
<dd>Specifies whether there is a run time limit on kernels </dd>
<dt><span class="enum-member-name-def">cudaDevAttrIntegrated = <span class="ph ph apiData">18</span></span></dt>
<dd>Device is integrated with host memory </dd>
<dt><span class="enum-member-name-def">cudaDevAttrCanMapHostMemory = <span class="ph ph apiData">19</span></span></dt>
<dd>Device can map host memory into CUDA address space </dd>
<dt><span class="enum-member-name-def">cudaDevAttrComputeMode = <span class="ph ph apiData">20</span></span></dt>
<dd>Compute mode (See <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g7eb25f5413a962faad0956d92bae10d0" shape="rect">cudaComputeMode</a> for details)
</dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DWidth = <span class="ph ph apiData">21</span></span></dt>
<dd>Maximum 1D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DWidth = <span class="ph ph apiData">22</span></span></dt>
<dd>Maximum 2D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DHeight = <span class="ph ph apiData">23</span></span></dt>
<dd>Maximum 2D texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DWidth = <span class="ph ph apiData">24</span></span></dt>
<dd>Maximum 3D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DHeight = <span class="ph ph apiData">25</span></span></dt>
<dd>Maximum 3D texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DDepth = <span class="ph ph apiData">26</span></span></dt>
<dd>Maximum 3D texture depth </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLayeredWidth = <span class="ph ph apiData">27</span></span></dt>
<dd>Maximum 2D layered texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLayeredHeight = <span class="ph ph apiData">28</span></span></dt>
<dd>Maximum 2D layered texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLayeredLayers = <span class="ph ph apiData">29</span></span></dt>
<dd>Maximum layers in a 2D layered texture </dd>
<dt><span class="enum-member-name-def">cudaDevAttrSurfaceAlignment = <span class="ph ph apiData">30</span></span></dt>
<dd>Alignment requirement for surfaces </dd>
<dt><span class="enum-member-name-def">cudaDevAttrConcurrentKernels = <span class="ph ph apiData">31</span></span></dt>
<dd>Device can possibly execute multiple kernels concurrently </dd>
<dt><span class="enum-member-name-def">cudaDevAttrEccEnabled = <span class="ph ph apiData">32</span></span></dt>
<dd>Device has ECC support enabled </dd>
<dt><span class="enum-member-name-def">cudaDevAttrPciBusId = <span class="ph ph apiData">33</span></span></dt>
<dd>PCI bus ID of the device </dd>
<dt><span class="enum-member-name-def">cudaDevAttrPciDeviceId = <span class="ph ph apiData">34</span></span></dt>
<dd>PCI device ID of the device </dd>
<dt><span class="enum-member-name-def">cudaDevAttrTccDriver = <span class="ph ph apiData">35</span></span></dt>
<dd>Device is using TCC driver model </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMemoryClockRate = <span class="ph ph apiData">36</span></span></dt>
<dd>Peak memory clock frequency in kilohertz </dd>
<dt><span class="enum-member-name-def">cudaDevAttrGlobalMemoryBusWidth = <span class="ph ph apiData">37</span></span></dt>
<dd>Global memory bus width in bits </dd>
<dt><span class="enum-member-name-def">cudaDevAttrL2CacheSize = <span class="ph ph apiData">38</span></span></dt>
<dd>Size of L2 cache in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxThreadsPerMultiProcessor = <span class="ph ph apiData">39</span></span></dt>
<dd>Maximum resident threads per multiprocessor </dd>
<dt><span class="enum-member-name-def">cudaDevAttrAsyncEngineCount = <span class="ph ph apiData">40</span></span></dt>
<dd>Number of asynchronous engines </dd>
<dt><span class="enum-member-name-def">cudaDevAttrUnifiedAddressing = <span class="ph ph apiData">41</span></span></dt>
<dd>Device shares a unified address space with the host </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DLayeredWidth = <span class="ph ph apiData">42</span></span></dt>
<dd>Maximum 1D layered texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DLayeredLayers = <span class="ph ph apiData">43</span></span></dt>
<dd>Maximum layers in a 1D layered texture </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DGatherWidth = <span class="ph ph apiData">45</span></span></dt>
<dd>Maximum 2D texture width if cudaArrayTextureGather is set </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DGatherHeight = <span class="ph ph apiData">46</span></span></dt>
<dd>Maximum 2D texture height if cudaArrayTextureGather is set </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DWidthAlt = <span class="ph ph apiData">47</span></span></dt>
<dd>Alternate maximum 3D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DHeightAlt = <span class="ph ph apiData">48</span></span></dt>
<dd>Alternate maximum 3D texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DDepthAlt = <span class="ph ph apiData">49</span></span></dt>
<dd>Alternate maximum 3D texture depth </dd>
<dt><span class="enum-member-name-def">cudaDevAttrPciDomainId = <span class="ph ph apiData">50</span></span></dt>
<dd>PCI domain ID of the device </dd>
<dt><span class="enum-member-name-def">cudaDevAttrTexturePitchAlignment = <span class="ph ph apiData">51</span></span></dt>
<dd>Pitch alignment requirement for textures </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTextureCubemapWidth = <span class="ph ph apiData">52</span></span></dt>
<dd>Maximum cubemap texture width/height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTextureCubemapLayeredWidth = <span class="ph ph apiData">53</span></span></dt>
<dd>Maximum cubemap layered texture width/height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTextureCubemapLayeredLayers = <span class="ph ph apiData">54</span></span></dt>
<dd>Maximum layers in a cubemap layered texture </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface1DWidth = <span class="ph ph apiData">55</span></span></dt>
<dd>Maximum 1D surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DWidth = <span class="ph ph apiData">56</span></span></dt>
<dd>Maximum 2D surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DHeight = <span class="ph ph apiData">57</span></span></dt>
<dd>Maximum 2D surface height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface3DWidth = <span class="ph ph apiData">58</span></span></dt>
<dd>Maximum 3D surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface3DHeight = <span class="ph ph apiData">59</span></span></dt>
<dd>Maximum 3D surface height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface3DDepth = <span class="ph ph apiData">60</span></span></dt>
<dd>Maximum 3D surface depth </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface1DLayeredWidth = <span class="ph ph apiData">61</span></span></dt>
<dd>Maximum 1D layered surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface1DLayeredLayers = <span class="ph ph apiData">62</span></span></dt>
<dd>Maximum layers in a 1D layered surface </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DLayeredWidth = <span class="ph ph apiData">63</span></span></dt>
<dd>Maximum 2D layered surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DLayeredHeight = <span class="ph ph apiData">64</span></span></dt>
<dd>Maximum 2D layered surface height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DLayeredLayers = <span class="ph ph apiData">65</span></span></dt>
<dd>Maximum layers in a 2D layered surface </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurfaceCubemapWidth = <span class="ph ph apiData">66</span></span></dt>
<dd>Maximum cubemap surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurfaceCubemapLayeredWidth = <span class="ph ph apiData">67</span></span></dt>
<dd>Maximum cubemap layered surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurfaceCubemapLayeredLayers = <span class="ph ph apiData">68</span></span></dt>
<dd>Maximum layers in a cubemap layered surface </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DLinearWidth = <span class="ph ph apiData">69</span></span></dt>
<dd>Maximum 1D linear texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLinearWidth = <span class="ph ph apiData">70</span></span></dt>
<dd>Maximum 2D linear texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLinearHeight = <span class="ph ph apiData">71</span></span></dt>
<dd>Maximum 2D linear texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLinearPitch = <span class="ph ph apiData">72</span></span></dt>
<dd>Maximum 2D linear texture pitch in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DMipmappedWidth = <span class="ph ph apiData">73</span></span></dt>
<dd>Maximum mipmapped 2D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DMipmappedHeight = <span class="ph ph apiData">74</span></span></dt>
<dd>Maximum mipmapped 2D texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrComputeCapabilityMajor = <span class="ph ph apiData">75</span></span></dt>
<dd>Major compute capability version number </dd>
<dt><span class="enum-member-name-def">cudaDevAttrComputeCapabilityMinor = <span class="ph ph apiData">76</span></span></dt>
<dd>Minor compute capability version number </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DMipmappedWidth = <span class="ph ph apiData">77</span></span></dt>
<dd>Maximum mipmapped 1D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrStreamPrioritiesSupported = <span class="ph ph apiData">78</span></span></dt>
<dd>Device supports stream priorities </dd>
<dt><span class="enum-member-name-def">cudaDevAttrGlobalL1CacheSupported = <span class="ph ph apiData">79</span></span></dt>
<dd>Device supports caching globals in L1 </dd>
<dt><span class="enum-member-name-def">cudaDevAttrLocalL1CacheSupported = <span class="ph ph apiData">80</span></span></dt>
<dd>Device supports caching locals in L1 </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSharedMemoryPerMultiprocessor = <span class="ph ph apiData">81</span></span></dt>
<dd>Maximum shared memory available per multiprocessor in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxRegistersPerMultiprocessor = <span class="ph ph apiData">82</span></span></dt>
<dd>Maximum number of 32-bit registers available per multiprocessor </dd>
<dt><span class="enum-member-name-def">cudaDevAttrManagedMemory = <span class="ph ph apiData">83</span></span></dt>
<dd>Device can allocate managed memory on this system </dd>
<dt><span class="enum-member-name-def">cudaDevAttrIsMultiGpuBoard = <span class="ph ph apiData">84</span></span></dt>
<dd>Device is on a multi-GPU board </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMultiGpuBoardGroupID = <span class="ph ph apiData">85</span></span></dt>
<dd>Unique identifier for a group of devices on the same multi-GPU board </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" id="group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" shape="rect">
<!-- --></a><span>enum cudaError</span></dt>
<dd class="description">
<div class="section">
<p>CUDA error types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaSuccess = <span class="ph ph apiData">0</span></span></dt>
<dd>The API call returned with no errors. In the case of query calls, this can also mean that the operation being queried is complete
(see <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1gf8e4ddb569b1da032c060f0c54da698f" title="Queries an event's status." shape="rect">cudaEventQuery()</a> and <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1ge78feba9080b59fe0fff536a42c13e6d" title="Queries an asynchronous stream for completion status." shape="rect">cudaStreamQuery()</a>).
</dd>
<dt><span class="enum-member-name-def">cudaErrorMissingConfiguration = <span class="ph ph apiData">1</span></span></dt>
<dd>The device function being invoked (usually via <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gf4f3215d06b6d90849a3d977f9440002" title="Launches a device function." shape="rect">cudaLaunch()</a>) was not previously configured via the <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall()</a> function.
</dd>
<dt><span class="enum-member-name-def">cudaErrorMemoryAllocation = <span class="ph ph apiData">2</span></span></dt>
<dd>The API call failed because it was unable to allocate enough memory to perform the requested operation. </dd>
<dt><span class="enum-member-name-def">cudaErrorInitializationError = <span class="ph ph apiData">3</span></span></dt>
<dd>The API call failed because the CUDA driver and runtime could not be initialized. </dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchFailure = <span class="ph ph apiData">4</span></span></dt>
<dd>An exception occurred on the device while executing a kernel. Common causes include dereferencing an invalid device pointer
and accessing out of bounds shared memory. The device cannot be used until <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" title="Exit and clean up from CUDA launches." shape="rect">cudaThreadExit()</a> is called. All existing device memory allocations are invalid and must be reconstructed if the program is to continue using
CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorPriorLaunchFailure = <span class="ph ph apiData">5</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000040" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that a previous kernel launch failed. This was previously used for device emulation of kernel launches.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchTimeout = <span class="ph ph apiData">6</span></span></dt>
<dd>This indicates that the device kernel took too long to execute. This can only occur if timeouts are enabled - see the device
property <a class="xref" href="structcudaDeviceProp.html#structcudaDeviceProp_19a63114766c4d2309f00403c1bf056c8" shape="rect">kernelExecTimeoutEnabled</a> for more information. The device cannot be used until <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" title="Exit and clean up from CUDA launches." shape="rect">cudaThreadExit()</a> is called. All existing device memory allocations are invalid and must be reconstructed if the program is to continue using
CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchOutOfResources = <span class="ph ph apiData">7</span></span></dt>
<dd>This indicates that a launch did not occur because it did not have appropriate resources. Although this error is similar to
<a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038d3934977826b2e1488dfeb7e0614e776" shape="rect">cudaErrorInvalidConfiguration</a>, this error usually indicates that the user has attempted to pass too many arguments to the device kernel, or the kernel
launch specifies too many threads for the kernel's register count.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidDeviceFunction = <span class="ph ph apiData">8</span></span></dt>
<dd>The requested device function does not exist or is not compiled for the proper device architecture. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidConfiguration = <span class="ph ph apiData">9</span></span></dt>
<dd>This indicates that a kernel launch is requesting resources that can never be satisfied by the current device. Requesting
more shared memory per block than the device supports will trigger this error, as will requesting too many threads or blocks.
See <a class="xref" href="structcudaDeviceProp.html#structcudaDeviceProp" shape="rect">cudaDeviceProp</a> for more device limitations.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidDevice = <span class="ph ph apiData">10</span></span></dt>
<dd>This indicates that the device ordinal supplied by the user does not correspond to a valid CUDA device. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidValue = <span class="ph ph apiData">11</span></span></dt>
<dd>This indicates that one or more of the parameters passed to the API call is not within an acceptable range of values. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidPitchValue = <span class="ph ph apiData">12</span></span></dt>
<dd>This indicates that one or more of the pitch-related parameters passed to the API call is not within the acceptable range
for pitch.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidSymbol = <span class="ph ph apiData">13</span></span></dt>
<dd>This indicates that the symbol name/identifier passed to the API call is not a valid name or identifier. </dd>
<dt><span class="enum-member-name-def">cudaErrorMapBufferObjectFailed = <span class="ph ph apiData">14</span></span></dt>
<dd>This indicates that the buffer object could not be mapped. </dd>
<dt><span class="enum-member-name-def">cudaErrorUnmapBufferObjectFailed = <span class="ph ph apiData">15</span></span></dt>
<dd>This indicates that the buffer object could not be unmapped. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidHostPointer = <span class="ph ph apiData">16</span></span></dt>
<dd>This indicates that at least one host pointer passed to the API call is not a valid host pointer. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidDevicePointer = <span class="ph ph apiData">17</span></span></dt>
<dd>This indicates that at least one device pointer passed to the API call is not a valid device pointer. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidTexture = <span class="ph ph apiData">18</span></span></dt>
<dd>This indicates that the texture passed to the API call is not a valid texture. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidTextureBinding = <span class="ph ph apiData">19</span></span></dt>
<dd>This indicates that the texture binding is not valid. This occurs if you call <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g6076c6bf0b1f2e52a36cd51af9d78fb4" title="Get the alignment offset of a texture." shape="rect">cudaGetTextureAlignmentOffset()</a> with an unbound texture.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidChannelDescriptor = <span class="ph ph apiData">20</span></span></dt>
<dd>This indicates that the channel descriptor passed to the API call is not valid. This occurs if the format is not one of the
formats specified by <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" shape="rect">cudaChannelFormatKind</a>, or if one of the dimensions is invalid.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidMemcpyDirection = <span class="ph ph apiData">21</span></span></dt>
<dd>This indicates that the direction of the memcpy passed to the API call is not one of the types specified by <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" shape="rect">cudaMemcpyKind</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorAddressOfConstant = <span class="ph ph apiData">22</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000041" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Variables in constant memory may now have their address taken by the runtime
via <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g1b2a5ca2b220e77deb6a777bf3f75a65" title="Finds the address associated with a CUDA symbol." shape="rect">cudaGetSymbolAddress()</a>. </span></p>
<p>This indicated that the user has taken the address of a constant variable, which was forbidden up until the CUDA 3.1 release.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorTextureFetchFailed = <span class="ph ph apiData">23</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000042" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that a texture fetch was not able to be performed. This was previously used for device emulation of texture
operations.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorTextureNotBound = <span class="ph ph apiData">24</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000043" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that a texture was not bound for access. This was previously used for device emulation of texture operations.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorSynchronizationError = <span class="ph ph apiData">25</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000044" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that a synchronization operation had failed. This was previously used for some device emulation functions.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidFilterSetting = <span class="ph ph apiData">26</span></span></dt>
<dd>This indicates that a non-float texture was being accessed with linear filtering. This is not supported by CUDA. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidNormSetting = <span class="ph ph apiData">27</span></span></dt>
<dd>This indicates that an attempt was made to read a non-float texture as a normalized float. This is not supported by CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorMixedDeviceExecution = <span class="ph ph apiData">28</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000045" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>Mixing of device and device emulation code was not allowed.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorCudartUnloading = <span class="ph ph apiData">29</span></span></dt>
<dd>This indicates that a CUDA Runtime API call cannot be executed because it is being called during process shut down, at a point
in time after CUDA driver has been unloaded.
</dd>
<dt><span class="enum-member-name-def">cudaErrorUnknown = <span class="ph ph apiData">30</span></span></dt>
<dd>This indicates that an unknown internal error has occurred. </dd>
<dt><span class="enum-member-name-def">cudaErrorNotYetImplemented = <span class="ph ph apiData">31</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000046" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 4.1. </span></p>
<p>This indicates that the API call is not yet implemented. Production releases of CUDA will never return this error.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorMemoryValueTooLarge = <span class="ph ph apiData">32</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000047" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that an emulated device pointer exceeded the 32-bit address range.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidResourceHandle = <span class="ph ph apiData">33</span></span></dt>
<dd>This indicates that a resource handle passed to the API call was not valid. Resource handles are opaque types like <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" shape="rect">cudaStream_t</a> and <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" shape="rect">cudaEvent_t</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorNotReady = <span class="ph ph apiData">34</span></span></dt>
<dd>This indicates that asynchronous operations issued previously have not completed yet. This result is not actually an error,
but must be indicated differently than <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a> (which indicates completion). Calls that may return this value include <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1gf8e4ddb569b1da032c060f0c54da698f" title="Queries an event's status." shape="rect">cudaEventQuery()</a> and <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1ge78feba9080b59fe0fff536a42c13e6d" title="Queries an asynchronous stream for completion status." shape="rect">cudaStreamQuery()</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInsufficientDriver = <span class="ph ph apiData">35</span></span></dt>
<dd>This indicates that the installed NVIDIA CUDA driver is older than the CUDA runtime library. This is not a supported configuration.
Users should install an updated NVIDIA display driver to allow the application to run.
</dd>
<dt><span class="enum-member-name-def">cudaErrorSetOnActiveProcess = <span class="ph ph apiData">36</span></span></dt>
<dd>This indicates that the user has called <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g5754b9d4e409b6cc0e252ba240d7468b" title="Set a list of devices that can be used for CUDA." shape="rect">cudaSetValidDevices()</a>, <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g18074e885b4d89f5a0fe1beab589e0c8" title="Sets flags to be used for device executions." shape="rect">cudaSetDeviceFlags()</a>, <a class="xref" href="group__CUDART__D3D9.html#group__CUDART__D3D9_1g3b7a9c5a5f249fa1f8fb5743304474b5" title="Sets the Direct3D 9 device to use for interoperability with a CUDA device." shape="rect">cudaD3D9SetDirect3DDevice()</a>, <a class="xref" href="group__CUDART__D3D10__DEPRECATED.html#group__CUDART__D3D10__DEPRECATED_1geec2934147774dd7a611df971a548675" title="Sets the Direct3D 10 device to use for interoperability with a CUDA device." shape="rect">cudaD3D10SetDirect3DDevice</a>, <a class="xref" href="group__CUDART__D3D11__DEPRECATED.html#group__CUDART__D3D11__DEPRECATED_1g447d066794c8070432514185d1326446" title="Sets the Direct3D 11 device to use for interoperability with a CUDA device." shape="rect">cudaD3D11SetDirect3DDevice()</a>, or <a class="xref" href="group__CUDART__VDPAU.html#group__CUDART__VDPAU_1g93a9727b90c526a3493918bceafcb3f7" title="Sets a CUDA device to use VDPAU interoperability." shape="rect">cudaVDPAUSetVDPAUDevice()</a> after initializing the CUDA runtime by calling non-device management operations (allocating memory and launching kernels
are examples of non-device management operations). This error can also be returned if using runtime/driver interoperability
and there is an existing CUcontext active on the host thread.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidSurface = <span class="ph ph apiData">37</span></span></dt>
<dd>This indicates that the surface passed to the API call is not a valid surface. </dd>
<dt><span class="enum-member-name-def">cudaErrorNoDevice = <span class="ph ph apiData">38</span></span></dt>
<dd>This indicates that no CUDA-capable devices were detected by the installed CUDA driver. </dd>
<dt><span class="enum-member-name-def">cudaErrorECCUncorrectable = <span class="ph ph apiData">39</span></span></dt>
<dd>This indicates that an uncorrectable ECC error was detected during execution. </dd>
<dt><span class="enum-member-name-def">cudaErrorSharedObjectSymbolNotFound = <span class="ph ph apiData">40</span></span></dt>
<dd>This indicates that a link to a shared object failed to resolve. </dd>
<dt><span class="enum-member-name-def">cudaErrorSharedObjectInitFailed = <span class="ph ph apiData">41</span></span></dt>
<dd>This indicates that initialization of a shared object failed. </dd>
<dt><span class="enum-member-name-def">cudaErrorUnsupportedLimit = <span class="ph ph apiData">42</span></span></dt>
<dd>This indicates that the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" shape="rect">cudaLimit</a> passed to the API call is not supported by the active device.
</dd>
<dt><span class="enum-member-name-def">cudaErrorDuplicateVariableName = <span class="ph ph apiData">43</span></span></dt>
<dd>This indicates that multiple global or constant variables (across separate CUDA source files in the application) share the
same string name.
</dd>
<dt><span class="enum-member-name-def">cudaErrorDuplicateTextureName = <span class="ph ph apiData">44</span></span></dt>
<dd>This indicates that multiple textures (across separate CUDA source files in the application) share the same string name. </dd>
<dt><span class="enum-member-name-def">cudaErrorDuplicateSurfaceName = <span class="ph ph apiData">45</span></span></dt>
<dd>This indicates that multiple surfaces (across separate CUDA source files in the application) share the same string name. </dd>
<dt><span class="enum-member-name-def">cudaErrorDevicesUnavailable = <span class="ph ph apiData">46</span></span></dt>
<dd>This indicates that all CUDA devices are busy or unavailable at the current time. Devices are often busy/unavailable due to
use of <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg7eb25f5413a962faad0956d92bae10d06965403d087b7f1153726c999bbc879c" shape="rect">cudaComputeModeExclusive</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg7eb25f5413a962faad0956d92bae10d0fc71b88518e4501544d6e65b5f3671b6" shape="rect">cudaComputeModeProhibited</a> or when long running CUDA kernels have filled up the GPU and are blocking new work from starting. They can also be unavailable
due to memory constraints on a device that already has active CUDA work being performed.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidKernelImage = <span class="ph ph apiData">47</span></span></dt>
<dd>This indicates that the device kernel image is invalid. </dd>
<dt><span class="enum-member-name-def">cudaErrorNoKernelImageForDevice = <span class="ph ph apiData">48</span></span></dt>
<dd>This indicates that there is no kernel image available that is suitable for the device. This can occur when a user specifies
code generation options for a particular CUDA source file that do not include the corresponding device configuration.
</dd>
<dt><span class="enum-member-name-def">cudaErrorIncompatibleDriverContext = <span class="ph ph apiData">49</span></span></dt>
<dd>This indicates that the current context is not compatible with this the CUDA Runtime. This can only occur if you are using
CUDA Runtime/Driver interoperability and have created an existing Driver context using the driver API. The Driver context
may be incompatible either because the Driver context was created using an older version of the API, because the Runtime API
call expects a primary driver context and the Driver context is not primary, or because the Driver context has been destroyed.
Please see <a class="xref" href="group__CUDART__DRIVER.html#group__CUDART__DRIVER" shape="rect">Interactions</a> with the CUDA Driver API" for more information.
</dd>
<dt><span class="enum-member-name-def">cudaErrorPeerAccessAlreadyEnabled = <span class="ph ph apiData">50</span></span></dt>
<dd>This error indicates that a call to <a class="xref" href="group__CUDART__PEER.html#group__CUDART__PEER_1g9e5ea65a18938c2b8715a5602105c306" title="Enables direct access to memory allocations on a peer device." shape="rect">cudaDeviceEnablePeerAccess()</a> is trying to re-enable peer addressing on from a context which has already had peer addressing enabled.
</dd>
<dt><span class="enum-member-name-def">cudaErrorPeerAccessNotEnabled = <span class="ph ph apiData">51</span></span></dt>
<dd>This error indicates that <a class="xref" href="group__CUDART__PEER.html#group__CUDART__PEER_1gae24fc50bd0f1ce7f69032f91bde87ac" title="Disables direct access to memory allocations on a peer device." shape="rect">cudaDeviceDisablePeerAccess()</a> is trying to disable peer addressing which has not been enabled yet via <a class="xref" href="group__CUDART__PEER.html#group__CUDART__PEER_1g9e5ea65a18938c2b8715a5602105c306" title="Enables direct access to memory allocations on a peer device." shape="rect">cudaDeviceEnablePeerAccess()</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorDeviceAlreadyInUse = <span class="ph ph apiData">54</span></span></dt>
<dd>This indicates that a call tried to access an exclusive-thread device that is already in use by a different thread. </dd>
<dt><span class="enum-member-name-def">cudaErrorProfilerDisabled = <span class="ph ph apiData">55</span></span></dt>
<dd>This indicates profiler is not initialized for this run. This can happen when the application is running with external profiling
tools like visual profiler.
</dd>
<dt><span class="enum-member-name-def">cudaErrorProfilerNotInitialized = <span class="ph ph apiData">56</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000048" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 5.0. It is no longer an error to attempt to enable/disable the profiling via <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1gde61d4a32c92d43d5d3f28847d89fe68" title="Enable profiling." shape="rect">cudaProfilerStart</a> or <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1gfbae1163a2c1086eac72e1908c2597f1" title="Disable profiling." shape="rect">cudaProfilerStop</a> without initialization. </span></p>
<p></p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorProfilerAlreadyStarted = <span class="ph ph apiData">57</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000049" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 5.0. It is no longer an error to call <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1gde61d4a32c92d43d5d3f28847d89fe68" title="Enable profiling." shape="rect">cudaProfilerStart()</a> when profiling is already enabled. </span></p>
<p></p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorProfilerAlreadyStopped = <span class="ph ph apiData">58</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000050" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 5.0. It is no longer an error to call <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1gfbae1163a2c1086eac72e1908c2597f1" title="Disable profiling." shape="rect">cudaProfilerStop()</a> when profiling is already disabled. </span></p>
<p></p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorAssert = <span class="ph ph apiData">59</span></span></dt>
<dd>An assert triggered in device code during kernel execution. The device cannot be used again until <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" title="Exit and clean up from CUDA launches." shape="rect">cudaThreadExit()</a> is called. All existing allocations are invalid and must be reconstructed if the program is to continue using CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorTooManyPeers = <span class="ph ph apiData">60</span></span></dt>
<dd>This error indicates that the hardware resources required to enable peer access have been exhausted for one or more of the
devices passed to cudaEnablePeerAccess().
</dd>
<dt><span class="enum-member-name-def">cudaErrorHostMemoryAlreadyRegistered = <span class="ph ph apiData">61</span></span></dt>
<dd>This error indicates that the memory range passed to <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g36b9fe28f547f28d23742e8c7cd18141" title="Registers an existing host memory range for use by CUDA." shape="rect">cudaHostRegister()</a> has already been registered.
</dd>
<dt><span class="enum-member-name-def">cudaErrorHostMemoryNotRegistered = <span class="ph ph apiData">62</span></span></dt>
<dd>This error indicates that the pointer passed to <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gc07b1312c60ca36c118e2ed71b192afe" title="Unregisters a memory range that was registered with cudaHostRegister." shape="rect">cudaHostUnregister()</a> does not correspond to any currently registered memory region.
</dd>
<dt><span class="enum-member-name-def">cudaErrorOperatingSystem = <span class="ph ph apiData">63</span></span></dt>
<dd>This error indicates that an OS call failed. </dd>
<dt><span class="enum-member-name-def">cudaErrorPeerAccessUnsupported = <span class="ph ph apiData">64</span></span></dt>
<dd>This error indicates that P2P access is not supported across the given devices. </dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchMaxDepthExceeded = <span class="ph ph apiData">65</span></span></dt>
<dd>This error indicates that a device runtime grid launch did not occur because the depth of the child grid would exceed the
maximum supported number of nested grid launches.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchFileScopedTex = <span class="ph ph apiData">66</span></span></dt>
<dd>This error indicates that a grid launch did not occur because the kernel uses file-scoped textures which are unsupported by
the device runtime. Kernels launched via the device runtime only support textures created with the Texture Object API's.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchFileScopedSurf = <span class="ph ph apiData">67</span></span></dt>
<dd>This error indicates that a grid launch did not occur because the kernel uses file-scoped surfaces which are unsupported by
the device runtime. Kernels launched via the device runtime only support surfaces created with the Surface Object API's.
</dd>
<dt><span class="enum-member-name-def">cudaErrorSyncDepthExceeded = <span class="ph ph apiData">68</span></span></dt>
<dd>This error indicates that a call to <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g32bdc6229081137acd3cba5da2897779" title="Wait for compute device to finish." shape="rect">cudaDeviceSynchronize</a> made from the device runtime failed because the call was made at grid depth greater than than either the default (2 levels
of grids) or user specified device limit <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365123c4900be4af436cb769e4c72d07be11" shape="rect">cudaLimitDevRuntimeSyncDepth</a>. To be able to synchronize on launched grids at a greater depth successfully, the maximum nested depth at which <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g32bdc6229081137acd3cba5da2897779" title="Wait for compute device to finish." shape="rect">cudaDeviceSynchronize</a> will be called must be specified with the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365123c4900be4af436cb769e4c72d07be11" shape="rect">cudaLimitDevRuntimeSyncDepth</a> limit to the <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gb8a22e29cc297634b0702db0b69f59e7" title="Set resource limits." shape="rect">cudaDeviceSetLimit</a> api before the host-side launch of a kernel using the device runtime. Keep in mind that additional levels of sync depth require
the runtime to reserve large amounts of device memory that cannot be used for user allocations.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchPendingCountExceeded = <span class="ph ph apiData">69</span></span></dt>
<dd>This error indicates that a device runtime grid launch failed because the launch would exceed the limit <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365118712cb05d2c3efaeea73afba823d916" shape="rect">cudaLimitDevRuntimePendingLaunchCount</a>. For this launch to proceed successfully, <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gb8a22e29cc297634b0702db0b69f59e7" title="Set resource limits." shape="rect">cudaDeviceSetLimit</a> must be called to set the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365118712cb05d2c3efaeea73afba823d916" shape="rect">cudaLimitDevRuntimePendingLaunchCount</a> to be higher than the upper bound of outstanding launches that can be issued to the device runtime. Keep in mind that raising
the limit of pending device runtime launches will require the runtime to reserve device memory that cannot be used for user
allocations.
</dd>
<dt><span class="enum-member-name-def">cudaErrorNotPermitted = <span class="ph ph apiData">70</span></span></dt>
<dd>This error indicates the attempted operation is not permitted. </dd>
<dt><span class="enum-member-name-def">cudaErrorNotSupported = <span class="ph ph apiData">71</span></span></dt>
<dd>This error indicates the attempted operation is not supported on the current system or device. </dd>
<dt><span class="enum-member-name-def">cudaErrorHardwareStackError = <span class="ph ph apiData">72</span></span></dt>
<dd>Device encountered an error in the call stack during kernel execution, possibly due to stack corruption or exceeding the stack
size limit. The context cannot be used, so it must be destroyed (and a new one should be created). All existing device memory
allocations from this context are invalid and must be reconstructed if the program is to continue using CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorIllegalInstruction = <span class="ph ph apiData">73</span></span></dt>
<dd>The device encountered an illegal instruction during kernel execution The context cannot be used, so it must be destroyed
(and a new one should be created). All existing device memory allocations from this context are invalid and must be reconstructed
if the program is to continue using CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorMisalignedAddress = <span class="ph ph apiData">74</span></span></dt>
<dd>The device encountered a load or store instruction on a memory address which is not aligned. The context cannot be used, so
it must be destroyed (and a new one should be created). All existing device memory allocations from this context are invalid
and must be reconstructed if the program is to continue using CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidAddressSpace = <span class="ph ph apiData">75</span></span></dt>
<dd>While executing a kernel, the device encountered an instruction which can only operate on memory locations in certain address
spaces (global, shared, or local), but was supplied a memory address not belonging to an allowed address space. The context
cannot be used, so it must be destroyed (and a new one should be created). All existing device memory allocations from this
context are invalid and must be reconstructed if the program is to continue using CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidPc = <span class="ph ph apiData">76</span></span></dt>
<dd>The device encountered an invalid program counter. The context cannot be used, so it must be destroyed (and a new one should
be created). All existing device memory allocations from this context are invalid and must be reconstructed if the program
is to continue using CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorIllegalAddress = <span class="ph ph apiData">77</span></span></dt>
<dd>The device encountered a load or store instruction on an invalid memory address. The context cannot be used, so it must be
destroyed (and a new one should be created). All existing device memory allocations from this context are invalid and must
be reconstructed if the program is to continue using CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidPtx = <span class="ph ph apiData">78</span></span></dt>
<dd>A PTX compilation failed. The runtime may fall back to compiling PTX if an application does not contain a suitable binary
for the current device.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidGraphicsContext = <span class="ph ph apiData">79</span></span></dt>
<dd>This indicates an error with the OpenGL or DirectX context. </dd>
<dt><span class="enum-member-name-def">cudaErrorStartupFailure = <span class="ph ph apiData">0x7f</span></span></dt>
<dd>This indicates an internal startup failure in the CUDA runtime. </dd>
<dt><span class="enum-member-name-def">cudaErrorApiFailureBase = <span class="ph ph apiData">10000</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000051" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 4.1. </span></p>
<p>Any unhandled CUDA driver error is added to this value and returned via the runtime. Production releases of CUDA should not
return such errors.
</p>
</dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" id="group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" shape="rect">
<!-- --></a><span>enum cudaFuncCache</span></dt>
<dd class="description">
<div class="section">
<p>CUDA function cache configurations </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaFuncCachePreferNone = <span class="ph ph apiData">0</span></span></dt>
<dd>Default function cache configuration, no preference </dd>
<dt><span class="enum-member-name-def">cudaFuncCachePreferShared = <span class="ph ph apiData">1</span></span></dt>
<dd>Prefer larger shared memory and smaller L1 cache </dd>
<dt><span class="enum-member-name-def">cudaFuncCachePreferL1 = <span class="ph ph apiData">2</span></span></dt>
<dd>Prefer larger L1 cache and smaller shared memory </dd>
<dt><span class="enum-member-name-def">cudaFuncCachePreferEqual = <span class="ph ph apiData">3</span></span></dt>
<dd>Prefer equal size L1 cache and shared memory </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbf3ce16a621826a09263b8a58902fee8" id="group__CUDART__TYPES_1gbf3ce16a621826a09263b8a58902fee8" shape="rect">
<!-- --></a><span>enum cudaGraphicsCubeFace</span></dt>
<dd class="description">
<div class="section">
<p>CUDA graphics interop array indices for cube maps </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaGraphicsCubeFacePositiveX = <span class="ph ph apiData">0x00</span></span></dt>
<dd>Positive X face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFaceNegativeX = <span class="ph ph apiData">0x01</span></span></dt>
<dd>Negative X face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFacePositiveY = <span class="ph ph apiData">0x02</span></span></dt>
<dd>Positive Y face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFaceNegativeY = <span class="ph ph apiData">0x03</span></span></dt>
<dd>Negative Y face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFacePositiveZ = <span class="ph ph apiData">0x04</span></span></dt>
<dd>Positive Z face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFaceNegativeZ = <span class="ph ph apiData">0x05</span></span></dt>
<dd>Negative Z face of cubemap </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g2c3c3a69caaf333d29d0b38b75de5ffd" id="group__CUDART__TYPES_1g2c3c3a69caaf333d29d0b38b75de5ffd" shape="rect">
<!-- --></a><span>enum cudaGraphicsMapFlags</span></dt>
<dd class="description">
<div class="section">
<p>CUDA graphics interop map flags </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaGraphicsMapFlagsNone = <span class="ph ph apiData">0</span></span></dt>
<dd>Default; Assume resource can be read/written </dd>
<dt><span class="enum-member-name-def">cudaGraphicsMapFlagsReadOnly = <span class="ph ph apiData">1</span></span></dt>
<dd>CUDA will not write to this resource </dd>
<dt><span class="enum-member-name-def">cudaGraphicsMapFlagsWriteDiscard = <span class="ph ph apiData">2</span></span></dt>
<dd>CUDA will only write to and will not read from this resource </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gd17cc29b28205bbe32ac575eba16c277" id="group__CUDART__TYPES_1gd17cc29b28205bbe32ac575eba16c277" shape="rect">
<!-- --></a><span>enum cudaGraphicsRegisterFlags</span></dt>
<dd class="description">
<div class="section">
<p>CUDA graphics interop register flags </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsNone = <span class="ph ph apiData">0</span></span></dt>
<dd>Default </dd>
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsReadOnly = <span class="ph ph apiData">1</span></span></dt>
<dd>CUDA will not write to this resource </dd>
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsWriteDiscard = <span class="ph ph apiData">2</span></span></dt>
<dd>CUDA will only write to and will not read from this resource </dd>
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsSurfaceLoadStore = <span class="ph ph apiData">4</span></span></dt>
<dd>CUDA will bind this resource to a surface reference </dd>
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsTextureGather = <span class="ph ph apiData">8</span></span></dt>
<dd>CUDA will perform texture gather operations on this resource </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" id="group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" shape="rect">
<!-- --></a><span>enum cudaLimit</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Limits </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaLimitStackSize = <span class="ph ph apiData">0x00</span></span></dt>
<dd>GPU thread stack size </dd>
<dt><span class="enum-member-name-def">cudaLimitPrintfFifoSize = <span class="ph ph apiData">0x01</span></span></dt>
<dd>GPU printf/fprintf FIFO size </dd>
<dt><span class="enum-member-name-def">cudaLimitMallocHeapSize = <span class="ph ph apiData">0x02</span></span></dt>
<dd>GPU malloc heap size </dd>
<dt><span class="enum-member-name-def">cudaLimitDevRuntimeSyncDepth = <span class="ph ph apiData">0x03</span></span></dt>
<dd>GPU device runtime synchronize depth </dd>
<dt><span class="enum-member-name-def">cudaLimitDevRuntimePendingLaunchCount = <span class="ph ph apiData">0x04</span></span></dt>
<dd>GPU device runtime pending launch count </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" id="group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" shape="rect">
<!-- --></a><span>enum cudaMemcpyKind</span></dt>
<dd class="description">
<div class="section">
<p>CUDA memory copy types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaMemcpyHostToHost = <span class="ph ph apiData">0</span></span></dt>
<dd>Host -> Host </dd>
<dt><span class="enum-member-name-def">cudaMemcpyHostToDevice = <span class="ph ph apiData">1</span></span></dt>
<dd>Host -> Device </dd>
<dt><span class="enum-member-name-def">cudaMemcpyDeviceToHost = <span class="ph ph apiData">2</span></span></dt>
<dd>Device -> Host </dd>
<dt><span class="enum-member-name-def">cudaMemcpyDeviceToDevice = <span class="ph ph apiData">3</span></span></dt>
<dd>Device -> Device </dd>
<dt><span class="enum-member-name-def">cudaMemcpyDefault = <span class="ph ph apiData">4</span></span></dt>
<dd>Default based unified virtual address space </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g13de56a8fe75569530ecc3a3106e9b6d" id="group__CUDART__TYPES_1g13de56a8fe75569530ecc3a3106e9b6d" shape="rect">
<!-- --></a><span>enum cudaMemoryType</span></dt>
<dd class="description">
<div class="section">
<p>CUDA memory types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaMemoryTypeHost = <span class="ph ph apiData">1</span></span></dt>
<dd>Host memory </dd>
<dt><span class="enum-member-name-def">cudaMemoryTypeDevice = <span class="ph ph apiData">2</span></span></dt>
<dd>Device memory </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" id="group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" shape="rect">
<!-- --></a><span>enum cudaOutputMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Profiler Output modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaKeyValuePair = <span class="ph ph apiData">0x00</span></span></dt>
<dd>Output mode Key-Value pair format. </dd>
<dt><span class="enum-member-name-def">cudaCSV = <span class="ph ph apiData">0x01</span></span></dt>
<dd>Output mode Comma separated values format. </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g067b774c0e639817a00a972c8e2c203c" id="group__CUDART__TYPES_1g067b774c0e639817a00a972c8e2c203c" shape="rect">
<!-- --></a><span>enum cudaResourceType</span></dt>
<dd class="description">
<div class="section">
<p>CUDA resource types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaResourceTypeArray = <span class="ph ph apiData">0x00</span></span></dt>
<dd>Array resource </dd>
<dt><span class="enum-member-name-def">cudaResourceTypeMipmappedArray = <span class="ph ph apiData">0x01</span></span></dt>
<dd>Mipmapped array resource </dd>
<dt><span class="enum-member-name-def">cudaResourceTypeLinear = <span class="ph ph apiData">0x02</span></span></dt>
<dd>Linear resource </dd>
<dt><span class="enum-member-name-def">cudaResourceTypePitch2D = <span class="ph ph apiData">0x03</span></span></dt>
<dd>Pitch 2D resource </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6b3a50368a0aa592f65e928adca9b929" id="group__CUDART__TYPES_1g6b3a50368a0aa592f65e928adca9b929" shape="rect">
<!-- --></a><span>enum cudaResourceViewFormat</span></dt>
<dd class="description">
<div class="section">
<p>CUDA texture resource view formats </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaResViewFormatNone = <span class="ph ph apiData">0x00</span></span></dt>
<dd>No resource view format (use underlying resource format) </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedChar1 = <span class="ph ph apiData">0x01</span></span></dt>
<dd>1 channel unsigned 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedChar2 = <span class="ph ph apiData">0x02</span></span></dt>
<dd>2 channel unsigned 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedChar4 = <span class="ph ph apiData">0x03</span></span></dt>
<dd>4 channel unsigned 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedChar1 = <span class="ph ph apiData">0x04</span></span></dt>
<dd>1 channel signed 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedChar2 = <span class="ph ph apiData">0x05</span></span></dt>
<dd>2 channel signed 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedChar4 = <span class="ph ph apiData">0x06</span></span></dt>
<dd>4 channel signed 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedShort1 = <span class="ph ph apiData">0x07</span></span></dt>
<dd>1 channel unsigned 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedShort2 = <span class="ph ph apiData">0x08</span></span></dt>
<dd>2 channel unsigned 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedShort4 = <span class="ph ph apiData">0x09</span></span></dt>
<dd>4 channel unsigned 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedShort1 = <span class="ph ph apiData">0x0a</span></span></dt>
<dd>1 channel signed 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedShort2 = <span class="ph ph apiData">0x0b</span></span></dt>
<dd>2 channel signed 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedShort4 = <span class="ph ph apiData">0x0c</span></span></dt>
<dd>4 channel signed 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedInt1 = <span class="ph ph apiData">0x0d</span></span></dt>
<dd>1 channel unsigned 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedInt2 = <span class="ph ph apiData">0x0e</span></span></dt>
<dd>2 channel unsigned 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedInt4 = <span class="ph ph apiData">0x0f</span></span></dt>
<dd>4 channel unsigned 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedInt1 = <span class="ph ph apiData">0x10</span></span></dt>
<dd>1 channel signed 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedInt2 = <span class="ph ph apiData">0x11</span></span></dt>
<dd>2 channel signed 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedInt4 = <span class="ph ph apiData">0x12</span></span></dt>
<dd>4 channel signed 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatHalf1 = <span class="ph ph apiData">0x13</span></span></dt>
<dd>1 channel 16-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatHalf2 = <span class="ph ph apiData">0x14</span></span></dt>
<dd>2 channel 16-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatHalf4 = <span class="ph ph apiData">0x15</span></span></dt>
<dd>4 channel 16-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatFloat1 = <span class="ph ph apiData">0x16</span></span></dt>
<dd>1 channel 32-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatFloat2 = <span class="ph ph apiData">0x17</span></span></dt>
<dd>2 channel 32-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatFloat4 = <span class="ph ph apiData">0x18</span></span></dt>
<dd>4 channel 32-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed1 = <span class="ph ph apiData">0x19</span></span></dt>
<dd>Block compressed 1 </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed2 = <span class="ph ph apiData">0x1a</span></span></dt>
<dd>Block compressed 2 </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed3 = <span class="ph ph apiData">0x1b</span></span></dt>
<dd>Block compressed 3 </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed4 = <span class="ph ph apiData">0x1c</span></span></dt>
<dd>Block compressed 4 unsigned </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedBlockCompressed4 = <span class="ph ph apiData">0x1d</span></span></dt>
<dd>Block compressed 4 signed </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed5 = <span class="ph ph apiData">0x1e</span></span></dt>
<dd>Block compressed 5 unsigned </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedBlockCompressed5 = <span class="ph ph apiData">0x1f</span></span></dt>
<dd>Block compressed 5 signed </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed6H = <span class="ph ph apiData">0x20</span></span></dt>
<dd>Block compressed 6 unsigned half-float </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedBlockCompressed6H = <span class="ph ph apiData">0x21</span></span></dt>
<dd>Block compressed 6 signed half-float </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed7 = <span class="ph ph apiData">0x22</span></span></dt>
<dd>Block compressed 7 </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6e62d15f3c224625e8c9aa946f1709a6" id="group__CUDART__TYPES_1g6e62d15f3c224625e8c9aa946f1709a6" shape="rect">
<!-- --></a><span>enum cudaSharedMemConfig</span></dt>
<dd class="description">
<div class="section">
<p>CUDA shared memory configuration </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaSharedMemBankSizeDefault = <span class="ph ph apiData">0</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaSharedMemBankSizeFourByte = <span class="ph ph apiData">1</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaSharedMemBankSizeEightByte = <span class="ph ph apiData">2</span></span></dt>
<dd></dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gdc002e3c2a4fd592efa944e2c73a10fb" id="group__CUDART__TYPES_1gdc002e3c2a4fd592efa944e2c73a10fb" shape="rect">
<!-- --></a><span>enum cudaSurfaceBoundaryMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Surface boundary modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaBoundaryModeZero = <span class="ph ph apiData">0</span></span></dt>
<dd>Zero boundary mode </dd>
<dt><span class="enum-member-name-def">cudaBoundaryModeClamp = <span class="ph ph apiData">1</span></span></dt>
<dd>Clamp boundary mode </dd>
<dt><span class="enum-member-name-def">cudaBoundaryModeTrap = <span class="ph ph apiData">2</span></span></dt>
<dd>Trap boundary mode </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g427be57cb8aa90479139bba92267150f" id="group__CUDART__TYPES_1g427be57cb8aa90479139bba92267150f" shape="rect">
<!-- --></a><span>enum cudaSurfaceFormatMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Surface format modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaFormatModeForced = <span class="ph ph apiData">0</span></span></dt>
<dd>Forced format mode </dd>
<dt><span class="enum-member-name-def">cudaFormatModeAuto = <span class="ph ph apiData">1</span></span></dt>
<dd>Auto format mode </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g03e1bbd2c491d809279c7a47e2cd0351" id="group__CUDART__TYPES_1g03e1bbd2c491d809279c7a47e2cd0351" shape="rect">
<!-- --></a><span>enum cudaTextureAddressMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA texture address modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaAddressModeWrap = <span class="ph ph apiData">0</span></span></dt>
<dd>Wrapping address mode </dd>
<dt><span class="enum-member-name-def">cudaAddressModeClamp = <span class="ph ph apiData">1</span></span></dt>
<dd>Clamp to edge address mode </dd>
<dt><span class="enum-member-name-def">cudaAddressModeMirror = <span class="ph ph apiData">2</span></span></dt>
<dd>Mirror address mode </dd>
<dt><span class="enum-member-name-def">cudaAddressModeBorder = <span class="ph ph apiData">3</span></span></dt>
<dd>Border address mode </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gee4adb3d1b062cf05374de09325a82d5" id="group__CUDART__TYPES_1gee4adb3d1b062cf05374de09325a82d5" shape="rect">
<!-- --></a><span>enum cudaTextureFilterMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA texture filter modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaFilterModePoint = <span class="ph ph apiData">0</span></span></dt>
<dd>Point filter mode </dd>
<dt><span class="enum-member-name-def">cudaFilterModeLinear = <span class="ph ph apiData">1</span></span></dt>
<dd>Linear filter mode </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gd9266d02be93809558036ec4f3d5f43d" id="group__CUDART__TYPES_1gd9266d02be93809558036ec4f3d5f43d" shape="rect">
<!-- --></a><span>enum cudaTextureReadMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA texture read modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaReadModeElementType = <span class="ph ph apiData">0</span></span></dt>
<dd>Read texture as specified element type </dd>
<dt><span class="enum-member-name-def">cudaReadModeNormalizedFloat = <span class="ph ph apiData">1</span></span></dt>
<dd>Read texture as normalized float </dd>
</dl>
</div>
</dd>
</dl>
</div>
</div>
<hr id="contents-end"></hr>
</article>
</div>
</div>
<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/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>
<script type="text/javascript">var switchTo5x=true;</script><script type="text/javascript" src="http://w.sharethis.com/button/buttons.js"></script><script type="text/javascript">stLight.options({publisher: "998dc202-a267-4d8e-bce9-14debadb8d92", doNotHash: false, doNotCopy: false, hashAddressBar: false});</script></body>
</html>
distrib
>
Mageia
>
5
>
x86_64
>
media
>
nonfree-release
>
by-pkgid
>
d44b02ea46d82d6a48df31bbd1a088f3
>
files
>
1179
