<!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="C++ API Routines"></meta>
<meta name="abstract" content="C++-style interface built on top of CUDA runtime API."></meta>
<meta name="description" content=""></meta>
<meta name="DC.Format" content="XHTML"></meta>
<meta name="DC.Identifier" content="group__CUDART__HIGHLEVEL"></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____VERSION.html" shape="rect">< Previous</a> | <a href="group__CUDART__DRIVER.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__HIGHLEVEL"><a name="group__CUDART__HIGHLEVEL" shape="rect">
<!-- --></a><h2 class="topictitle2 cppModule">3.26. C++ API Routines</h2>
<div class="section">
<p>This section describes the C++ high level API functions of the CUDA runtime application programming interface. To use these
functions, your application needs to be compiled with the <tt class="ph tt code">nvcc</tt> compiler.
</p>
</div>
<h3 class="fake_sectiontitle member_header">Classes</h3>
<dl class="members">
<dt><span class="member_type">class </span><span class="member_name">
<div><a class="link" href="class____cudaOccupancyB2DHelper.html#class____cudaOccupancyB2DHelper" shape="rect">__cudaOccupancyB2DHelper</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="class____cudaOccupancyB2DHelper.html#class____cudaOccupancyB2DHelper" class="link" title="" shape="rect"></a></dd>
</dl>
<h3 class="fake_sectiontitle member_header">Functions</h3>
<dl class="members">
<dt><span class="template">template < class T, int dim ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g2871dc1e4e78b7b2f7e12bcba419d870" shape="rect">cudaBindSurfaceToArray</a> ( const surface < T, dim > &<span> </span><span class="keyword keyword apiItemName">surf</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" title="" shape="rect">cudaArray_const_t</a><span> </span><span class="keyword keyword apiItemName">array</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds an array to a surface </span></dd>
<dt><span class="template">template < class T, int dim ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g1ffeea0c649c7cb1328156aa21f00f1e" shape="rect">cudaBindSurfaceToArray</a> ( const surface < T, dim > &<span> </span><span class="keyword keyword apiItemName">surf</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" title="" shape="rect">cudaArray_const_t</a><span> </span><span class="keyword keyword apiItemName">array</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds an array to a surface </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" shape="rect">cudaBindTexture</a> ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, const void*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, size_t<span> </span><span class="keyword keyword apiItemName">size</span> = <span class="ph ph apiData">UINT_MAX</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds a memory area to a texture </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" shape="rect">cudaBindTexture</a> ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, const void*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span>, size_t<span> </span><span class="keyword keyword apiItemName">size</span> = <span class="ph ph apiData">UINT_MAX</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds a memory area to a texture </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" shape="rect">cudaBindTexture2D</a> ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, const void*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, size_t<span> </span><span class="keyword keyword apiItemName">width</span>, size_t<span> </span><span class="keyword keyword apiItemName">height</span>, size_t<span> </span><span class="keyword keyword apiItemName">pitch</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds a 2D memory area to a texture </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" shape="rect">cudaBindTexture2D</a> ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, const void*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span>, size_t<span> </span><span class="keyword keyword apiItemName">width</span>, size_t<span> </span><span class="keyword keyword apiItemName">height</span>, size_t<span> </span><span class="keyword keyword apiItemName">pitch</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds a 2D memory area to a texture </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" shape="rect">cudaBindTextureToArray</a> ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" title="" shape="rect">cudaArray_const_t</a><span> </span><span class="keyword keyword apiItemName">array</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds an array to a texture </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" shape="rect">cudaBindTextureToArray</a> ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" title="" shape="rect">cudaArray_const_t</a><span> </span><span class="keyword keyword apiItemName">array</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds an array to a texture </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g4073bc5299eb04bbd9340d996cde7c20" shape="rect">cudaBindTextureToMipmappedArray</a> ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" title="" shape="rect">cudaMipmappedArray_const_t</a><span> </span><span class="keyword keyword apiItemName">mipmappedArray</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds a mipmapped array to a texture </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g68b41d5065a43204ca5937eb41ae77d0" shape="rect">cudaBindTextureToMipmappedArray</a> ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" title="" shape="rect">cudaMipmappedArray_const_t</a><span> </span><span class="keyword keyword apiItemName">mipmappedArray</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Binds a mipmapped array to a texture </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" shape="rect">cudaCreateChannelDesc</a> ( void ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Returns a channel descriptor using the specified format </span></dd>
<dt><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1gb9774a7552ee76b564c8c650b083a86c" shape="rect">cudaEventCreate</a> ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" title="" shape="rect">cudaEvent_t</a>*<span> </span><span class="keyword keyword apiItemName">event</span>, unsigned int <span> </span><span class="keyword keyword apiItemName">flags</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Creates an event object with the specified flags </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g0b85e087210b47056cb6fc03a0e264e8" shape="rect">cudaFuncGetAttributes</a> ( <a href="structcudaFuncAttributes.html#structcudaFuncAttributes" title="" shape="rect">cudaFuncAttributes</a>*<span> </span><span class="keyword keyword apiItemName">attr</span>, T*<span> </span><span class="keyword keyword apiItemName">entry</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Find out attributes for a given function </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1ge0969184de8a5c2d809aa8d7d2425484" shape="rect">cudaFuncSetCacheConfig</a> ( T*<span> </span><span class="keyword keyword apiItemName">func</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" title="" shape="rect">cudaFuncCache</a><span> </span><span class="keyword keyword apiItemName">cacheConfig</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Sets the preferred cache configuration for a device function </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g5ca79fbb1f49f7fb8e45d768418c10f7" shape="rect">cudaGetSymbolAddress</a> ( void**<span> </span><span class="keyword keyword apiItemName">devPtr</span>, const T&<span> </span><span class="keyword keyword apiItemName">symbol</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Finds the address associated with a CUDA symbol </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g9b568e473b813e84aba99c44e6d57a90" shape="rect">cudaGetSymbolSize</a> ( size_t*<span> </span><span class="keyword keyword apiItemName">size</span>, const T&<span> </span><span class="keyword keyword apiItemName">symbol</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Finds the size of the object associated with a CUDA symbol </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" shape="rect">cudaGetTextureAlignmentOffset</a> ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Get the alignment offset of a texture </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1gf9f5de511075f30c1bf97ea4306e9728" shape="rect">cudaLaunch</a> ( T*<span> </span><span class="keyword keyword apiItemName">func</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Launches a device function </span></dd>
<dt><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1ge439496de696b166ba457dab5dd4f356" shape="rect">cudaMallocHost</a> ( void**<span> </span><span class="keyword keyword apiItemName">ptr</span>, size_t<span> </span><span class="keyword keyword apiItemName">size</span>, unsigned int <span> </span><span class="keyword keyword apiItemName">flags</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Allocates page-locked memory on the host </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" shape="rect">cudaMallocManaged</a> ( T**<span> </span><span class="keyword keyword apiItemName">devPtr</span>, size_t<span> </span><span class="keyword keyword apiItemName">size</span>, unsigned int <span> </span><span class="keyword keyword apiItemName">flags</span> = <span class="ph ph apiData">cudaMemAttachGlobal</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Allocates memory that will be automatically managed by the Unified Memory system. </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g6a9b39c2d139205e60c107c8f1802775" shape="rect">cudaMemcpyFromSymbol</a> ( void*<span> </span><span class="keyword keyword apiItemName">dst</span>, const T&<span> </span><span class="keyword keyword apiItemName">symbol</span>, size_t<span> </span><span class="keyword keyword apiItemName">count</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> = <span class="ph ph apiData">0</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" title="" shape="rect">cudaMemcpyKind</a><span> </span><span class="keyword keyword apiItemName">kind</span> = <span class="ph ph apiData">cudaMemcpyDeviceToHost</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Copies data from the given symbol on the device </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1ge8a47aa428b24d05e3a1bccff673a7c9" shape="rect">cudaMemcpyFromSymbolAsync</a> ( void*<span> </span><span class="keyword keyword apiItemName">dst</span>, const T&<span> </span><span class="keyword keyword apiItemName">symbol</span>, size_t<span> </span><span class="keyword keyword apiItemName">count</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> = <span class="ph ph apiData">0</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" title="" shape="rect">cudaMemcpyKind</a><span> </span><span class="keyword keyword apiItemName">kind</span> = <span class="ph ph apiData">cudaMemcpyDeviceToHost</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" title="" shape="rect">cudaStream_t</a><span> </span><span class="keyword keyword apiItemName">stream</span> = <span class="ph ph apiData">0</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Copies data from the given symbol on the device </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g0c15b63c7b065fda8998713831edcbc7" shape="rect">cudaMemcpyToSymbol</a> ( const T&<span> </span><span class="keyword keyword apiItemName">symbol</span>, const void*<span> </span><span class="keyword keyword apiItemName">src</span>, size_t<span> </span><span class="keyword keyword apiItemName">count</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> = <span class="ph ph apiData">0</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" title="" shape="rect">cudaMemcpyKind</a><span> </span><span class="keyword keyword apiItemName">kind</span> = <span class="ph ph apiData">cudaMemcpyHostToDevice</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Copies data to the given symbol on the device </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1gf04a6abff5155d11b12c35fe14a98280" shape="rect">cudaMemcpyToSymbolAsync</a> ( const T&<span> </span><span class="keyword keyword apiItemName">symbol</span>, const void*<span> </span><span class="keyword keyword apiItemName">src</span>, size_t<span> </span><span class="keyword keyword apiItemName">count</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> = <span class="ph ph apiData">0</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" title="" shape="rect">cudaMemcpyKind</a><span> </span><span class="keyword keyword apiItemName">kind</span> = <span class="ph ph apiData">cudaMemcpyHostToDevice</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" title="" shape="rect">cudaStream_t</a><span> </span><span class="keyword keyword apiItemName">stream</span> = <span class="ph ph apiData">0</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Copies data to the given symbol on the device </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1gec01149f3a448009f4198fcd810ffc8d" shape="rect">cudaOccupancyMaxActiveBlocksPerMultiprocessor</a> ( int*<span> </span><span class="keyword keyword apiItemName">numBlocks</span>, T<span> </span><span class="keyword keyword apiItemName">func</span>, int <span> </span><span class="keyword keyword apiItemName">blockSize</span>, size_t<span> </span><span class="keyword keyword apiItemName">dynamicSMemSize</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Returns occupancy for a device function. </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1gccd34d08d6ae77b0f61beed7afcf66d9" shape="rect">cudaOccupancyMaxPotentialBlockSize</a> ( int*<span> </span><span class="keyword keyword apiItemName">minGridSize</span>, int*<span> </span><span class="keyword keyword apiItemName">blockSize</span>, T<span> </span><span class="keyword keyword apiItemName">func</span>, size_t<span> </span><span class="keyword keyword apiItemName">dynamicSMemSize</span> = <span class="ph ph apiData">0</span>, int <span> </span><span class="keyword keyword apiItemName">blockSizeLimit</span> = <span class="ph ph apiData">0</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Returns grid and block size that achieves maximum potential occupancy for a device function. </span></dd>
<dt><span class="template">template < typename UnaryFunction, class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1gf69042ce23b8500b972fd74d2ae52bf0" shape="rect">cudaOccupancyMaxPotentialBlockSizeVariableSMem</a> ( int*<span> </span><span class="keyword keyword apiItemName">minGridSize</span>, int*<span> </span><span class="keyword keyword apiItemName">blockSize</span>, T<span> </span><span class="keyword keyword apiItemName">func</span>, UnaryFunction<span> </span><span class="keyword keyword apiItemName">blockSizeToDynamicSMemSize</span>, int <span> </span><span class="keyword keyword apiItemName">blockSizeLimit</span> = <span class="ph ph apiData">0</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Returns grid and block size that achieves maximum potential occupancy for a device function. </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g0ffbffed226005960c39688493c94c84" shape="rect">cudaSetupArgument</a> ( T<span> </span><span class="keyword keyword apiItemName">arg</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Configure a device launch </span></dd>
<dt><span class="template">template < class T ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1gebe68658a891edc398791a436a8e1d7c" shape="rect">cudaStreamAttachMemAsync</a> ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" title="" shape="rect">cudaStream_t</a><span> </span><span class="keyword keyword apiItemName">stream</span>, T*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, size_t<span> </span><span class="keyword keyword apiItemName">length</span> = <span class="ph ph apiData">0</span>, unsigned int <span> </span><span class="keyword keyword apiItemName">flags</span> = <span class="ph ph apiData">cudaMemAttachSingle</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">Attach memory to a stream asynchronously. </span></dd>
<dt><span class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></span><span class="member_type"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> </span><span class="member_name"><a href="#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" shape="rect">cudaUnbindTexture</a> ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc">[C++ API] Unbinds a texture </span></dd>
</dl>
<div class="description">
<h3 class="sectiontitle">Functions</h3>
<dl class="description">
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g2871dc1e4e78b7b2f7e12bcba419d870" id="group__CUDART__HIGHLEVEL_1g2871dc1e4e78b7b2f7e12bcba419d870" shape="rect">
<!-- --></a><p class="template">template < class T, int dim ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindSurfaceToArray ( const surface < T, dim > &<span> </span><span class="keyword keyword apiItemName">surf</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" title="" shape="rect">cudaArray_const_t</a><span> </span><span class="keyword keyword apiItemName">array</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds an array to a surface </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">surf</span></tt></dt>
<dd>- Surface to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">array</span></tt></dt>
<dd>- Memory array on device</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038aa711d1e9175231dc80eecb7b51936a3" shape="rect">cudaErrorInvalidSurface</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds the CUDA array <tt class="ph tt code">array</tt> to the surface reference <tt class="ph tt code">surf</tt>. The channel descriptor is inherited from the CUDA array. Any CUDA array previously bound to <tt class="ph tt code">surf</tt> is unbound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__SURFACE.html#group__CUDART__SURFACE_1ga2b349f6cf2299d564c21d4e6f0dd636" title="Binds an array to a surface." shape="rect">cudaBindSurfaceToArray ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1ffeea0c649c7cb1328156aa21f00f1e" title="[C++ API] Binds an array to a surface" shape="rect">cudaBindSurfaceToArray ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g1ffeea0c649c7cb1328156aa21f00f1e" id="group__CUDART__HIGHLEVEL_1g1ffeea0c649c7cb1328156aa21f00f1e" shape="rect">
<!-- --></a><p class="template">template < class T, int dim ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindSurfaceToArray ( const surface < T, dim > &<span> </span><span class="keyword keyword apiItemName">surf</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" title="" shape="rect">cudaArray_const_t</a><span> </span><span class="keyword keyword apiItemName">array</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds an array to a surface </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">surf</span></tt></dt>
<dd>- Surface to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">array</span></tt></dt>
<dd>- Memory array on device </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">desc</span></tt></dt>
<dd>- Channel format</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038aa711d1e9175231dc80eecb7b51936a3" shape="rect">cudaErrorInvalidSurface</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds the CUDA array <tt class="ph tt code">array</tt> to the surface reference <tt class="ph tt code">surf</tt>. <tt class="ph tt code">desc</tt> describes how the memory is interpreted when dealing with the surface. Any CUDA array previously bound to <tt class="ph tt code">surf</tt> is unbound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__SURFACE.html#group__CUDART__SURFACE_1ga2b349f6cf2299d564c21d4e6f0dd636" title="Binds an array to a surface." shape="rect">cudaBindSurfaceToArray ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2871dc1e4e78b7b2f7e12bcba419d870" title="[C++ API] Binds an array to a surface" shape="rect">cudaBindSurfaceToArray ( C++ API, inherited channel descriptor)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" id="group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindTexture ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, const void*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, size_t<span> </span><span class="keyword keyword apiItemName">size</span> = <span class="ph ph apiData">UINT_MAX</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds a memory area to a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">devPtr</span></tt></dt>
<dd>- Memory area on device </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">size</span></tt></dt>
<dd>- Size of the memory area pointed to by devPtr</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds <tt class="ph tt code">size</tt> bytes of the memory area pointed to by <tt class="ph tt code">devPtr</tt> to texture reference <tt class="ph tt code">tex</tt>. The channel descriptor is inherited from the texture reference type. The <tt class="ph tt code">offset</tt> parameter is an optional byte offset as with the low-level <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g3ea5f64f8e1255f2adfa393e0b4a7622" title="Binds a memory area to a texture." shape="rect">cudaBindTexture( size_t*, const struct textureReference*, const void*, const struct cudaChannelFormatDesc*, size_t)</a> function. Any memory previously bound to <tt class="ph tt code">tex</tt> is unbound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g3ea5f64f8e1255f2adfa393e0b4a7622" title="Binds a memory area to a texture." shape="rect">cudaBindTexture ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" id="group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindTexture ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, const void*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span>, size_t<span> </span><span class="keyword keyword apiItemName">size</span> = <span class="ph ph apiData">UINT_MAX</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds a memory area to a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">devPtr</span></tt></dt>
<dd>- Memory area on device </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">desc</span></tt></dt>
<dd>- Channel format </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">size</span></tt></dt>
<dd>- Size of the memory area pointed to by devPtr</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds <tt class="ph tt code">size</tt> bytes of the memory area pointed to by <tt class="ph tt code">devPtr</tt> to texture reference <tt class="ph tt code">tex</tt>. <tt class="ph tt code">desc</tt> describes how the memory is interpreted when fetching values from the texture. The <tt class="ph tt code">offset</tt> parameter is an optional byte offset as with the low-level <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g3ea5f64f8e1255f2adfa393e0b4a7622" title="Binds a memory area to a texture." shape="rect">cudaBindTexture()</a> function. Any memory previously bound to <tt class="ph tt code">tex</tt> is unbound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g3ea5f64f8e1255f2adfa393e0b4a7622" title="Binds a memory area to a texture." shape="rect">cudaBindTexture ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" id="group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindTexture2D ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, const void*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, size_t<span> </span><span class="keyword keyword apiItemName">width</span>, size_t<span> </span><span class="keyword keyword apiItemName">height</span>, size_t<span> </span><span class="keyword keyword apiItemName">pitch</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds a 2D memory area to a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture reference to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">devPtr</span></tt></dt>
<dd>- 2D memory area on device </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">width</span></tt></dt>
<dd>- Width in texel units </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">height</span></tt></dt>
<dd>- Height in texel units </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">pitch</span></tt></dt>
<dd>- Pitch in bytes</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds the 2D memory area pointed to by <tt class="ph tt code">devPtr</tt> to the texture reference <tt class="ph tt code">tex</tt>. The size of the area is constrained by <tt class="ph tt code">width</tt> in texel units, <tt class="ph tt code">height</tt> in texel units, and <tt class="ph tt code">pitch</tt> in byte units. The channel descriptor is inherited from the texture reference type. Any memory previously bound to <tt class="ph tt code">tex</tt> is unbound.
</p>
<p class="p">Since the hardware enforces an alignment requirement on texture base addresses, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D()</a> returns in <tt class="ph tt code">*offset</tt> a byte offset that must be applied to texture fetches in order to read from the desired memory. This offset must be divided
by the texel size and passed to kernels that read from the texture so they can be applied to the tex2D() function. If the
device memory pointer was returned from <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g16a37ee003fcd9374ac8e6a5d4dee29e" title="Allocate memory on the device." shape="rect">cudaMalloc()</a>, the offset is guaranteed to be 0 and NULL may be passed as the <tt class="ph tt code">offset</tt> parameter.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1gdc3ad1bb212e76043659f7e57a5ffba6" title="Binds a 2D memory area to a texture." shape="rect">cudaBindTexture2D ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" id="group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindTexture2D ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, const void*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span>, size_t<span> </span><span class="keyword keyword apiItemName">width</span>, size_t<span> </span><span class="keyword keyword apiItemName">height</span>, size_t<span> </span><span class="keyword keyword apiItemName">pitch</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds a 2D memory area to a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture reference to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">devPtr</span></tt></dt>
<dd>- 2D memory area on device </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">desc</span></tt></dt>
<dd>- Channel format </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">width</span></tt></dt>
<dd>- Width in texel units </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">height</span></tt></dt>
<dd>- Height in texel units </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">pitch</span></tt></dt>
<dd>- Pitch in bytes</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds the 2D memory area pointed to by <tt class="ph tt code">devPtr</tt> to the texture reference <tt class="ph tt code">tex</tt>. The size of the area is constrained by <tt class="ph tt code">width</tt> in texel units, <tt class="ph tt code">height</tt> in texel units, and <tt class="ph tt code">pitch</tt> in byte units. <tt class="ph tt code">desc</tt> describes how the memory is interpreted when fetching values from the texture. Any memory previously bound to <tt class="ph tt code">tex</tt> is unbound.
</p>
<p class="p">Since the hardware enforces an alignment requirement on texture base addresses, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D()</a> returns in <tt class="ph tt code">*offset</tt> a byte offset that must be applied to texture fetches in order to read from the desired memory. This offset must be divided
by the texel size and passed to kernels that read from the texture so they can be applied to the tex2D() function. If the
device memory pointer was returned from <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g16a37ee003fcd9374ac8e6a5d4dee29e" title="Allocate memory on the device." shape="rect">cudaMalloc()</a>, the offset is guaranteed to be 0 and NULL may be passed as the <tt class="ph tt code">offset</tt> parameter.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1gdc3ad1bb212e76043659f7e57a5ffba6" title="Binds a 2D memory area to a texture." shape="rect">cudaBindTexture2D ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" id="group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindTextureToArray ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" title="" shape="rect">cudaArray_const_t</a><span> </span><span class="keyword keyword apiItemName">array</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds an array to a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">array</span></tt></dt>
<dd>- Memory array on device</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds the CUDA array <tt class="ph tt code">array</tt> to the texture reference <tt class="ph tt code">tex</tt>. The channel descriptor is inherited from the CUDA array. Any CUDA array previously bound to <tt class="ph tt code">tex</tt> is unbound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1gff3725e968d267331c466530ed297227" title="Binds an array to a texture." shape="rect">cudaBindTextureToArray ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" id="group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindTextureToArray ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" title="" shape="rect">cudaArray_const_t</a><span> </span><span class="keyword keyword apiItemName">array</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds an array to a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">array</span></tt></dt>
<dd>- Memory array on device </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">desc</span></tt></dt>
<dd>- Channel format</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds the CUDA array <tt class="ph tt code">array</tt> to the texture reference <tt class="ph tt code">tex</tt>. <tt class="ph tt code">desc</tt> describes how the memory is interpreted when fetching values from the texture. Any CUDA array previously bound to <tt class="ph tt code">tex</tt> is unbound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1gff3725e968d267331c466530ed297227" title="Binds an array to a texture." shape="rect">cudaBindTextureToArray ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g4073bc5299eb04bbd9340d996cde7c20" id="group__CUDART__HIGHLEVEL_1g4073bc5299eb04bbd9340d996cde7c20" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindTextureToMipmappedArray ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" title="" shape="rect">cudaMipmappedArray_const_t</a><span> </span><span class="keyword keyword apiItemName">mipmappedArray</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds a mipmapped array to a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">mipmappedArray</span></tt></dt>
<dd>- Memory mipmapped array on device</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds the CUDA mipmapped array <tt class="ph tt code">mipmappedArray</tt> to the texture reference <tt class="ph tt code">tex</tt>. The channel descriptor is inherited from the CUDA array. Any CUDA mipmapped array previously bound to <tt class="ph tt code">tex</tt> is unbound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1gff3725e968d267331c466530ed297227" title="Binds an array to a texture." shape="rect">cudaBindTextureToArray ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g68b41d5065a43204ca5937eb41ae77d0" id="group__CUDART__HIGHLEVEL_1g68b41d5065a43204ca5937eb41ae77d0" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaBindTextureToMipmappedArray ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" title="" shape="rect">cudaMipmappedArray_const_t</a><span> </span><span class="keyword keyword apiItemName">mipmappedArray</span>, const <a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a>&<span> </span><span class="keyword keyword apiItemName">desc</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Binds a mipmapped array to a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture to bind </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">mipmappedArray</span></tt></dt>
<dd>- Memory mipmapped array on device </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">desc</span></tt></dt>
<dd>- Channel format</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Binds the CUDA mipmapped array <tt class="ph tt code">mipmappedArray</tt> to the texture reference <tt class="ph tt code">tex</tt>. <tt class="ph tt code">desc</tt> describes how the memory is interpreted when fetching values from the texture. Any CUDA mipmapped array previously bound
to <tt class="ph tt code">tex</tt> is unbound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1gff3725e968d267331c466530ed297227" title="Binds an array to a texture." shape="rect">cudaBindTextureToArray ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" id="group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" title="" shape="rect">cudaChannelFormatDesc</a> cudaCreateChannelDesc ( void ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Returns a channel descriptor using the specified format </div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return">Channel descriptor with format <tt class="ph tt code">f</tt></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Returns a channel descriptor with format <tt class="ph tt code">f</tt> and number of bits of each component <tt class="ph tt code">x</tt>, <tt class="ph tt code">y</tt>, <tt class="ph tt code">z</tt>, and <tt class="ph tt code">w</tt>. The <a class="xref" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" shape="rect">cudaChannelFormatDesc</a> is defined as: <pre xml:space="preserve">‎ struct <a class="xref" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" shape="rect">cudaChannelFormatDesc</a> {
int <a class="xref" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc_170dede802100e2acd9f334326e9d7926" shape="rect">x</a>, <a class="xref" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc_16570793c6567d0c704e8e8943ccaec43" shape="rect">y</a>, <a class="xref" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc_1e371d37d940d2397139b0a3b7302f51a" shape="rect">z</a>, <a class="xref" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc_106089c5a407a2cbd6ea05e5a39b19d69" shape="rect">w</a>;
enum <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" shape="rect">cudaChannelFormatKind</a>
<a class="xref" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc_17d561d361936688eeae79c3184698278" shape="rect">f</a>;
};</pre></p>
<p class="p">where <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" shape="rect">cudaChannelFormatKind</a> is one of <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg8085eac5cb54b4228f3619a60f235119943e8b95cd113175ac55c56d90b40ae0" shape="rect">cudaChannelFormatKindSigned</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg8085eac5cb54b4228f3619a60f235119240d73fa2dc05cbaa58f093f169ab3d4" shape="rect">cudaChannelFormatKindUnsigned</a>, or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg8085eac5cb54b4228f3619a60f2351191107be31913affb6b3b49d8a6e795ee0" shape="rect">cudaChannelFormatKindFloat</a>.
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g0ea6897bcf8184a501659dfefc58b563" title="Returns a channel descriptor using the specified format." shape="rect">cudaCreateChannelDesc ( Low level)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( High level)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( High level, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( High level)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( High level)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( High level, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( High level)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( High level)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1gb9774a7552ee76b564c8c650b083a86c" id="group__CUDART__HIGHLEVEL_1gb9774a7552ee76b564c8c650b083a86c" shape="rect">
<!-- --></a><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaEventCreate ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" title="" shape="rect">cudaEvent_t</a>*<span> </span><span class="keyword keyword apiItemName">event</span>, unsigned int <span> </span><span class="keyword keyword apiItemName">flags</span> ) </span></dt>
<dd class="description">
<div class="section">[C++ API] Creates an event object with the specified flags </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">event</span></tt></dt>
<dd>- Newly created event </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">flags</span></tt></dt>
<dd>- Flags for new event</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038ce7993a88ecf2c57b8102d55d997a18c" shape="rect">cudaErrorInitializationError</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038099def426efea2b2366d8d7ad09f974a" shape="rect">cudaErrorLaunchFailure</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038f210f50ae7f17f655e0504929606add9" shape="rect">cudaErrorMemoryAllocation</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Creates an event object with the specified flags. Valid flags include:
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g6f8811acffcc133b5e4a50de6646d18e" shape="rect">cudaEventDefault</a>: Default event creation flag.
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g26509a522be9d449aa7c8c279612452d" shape="rect">cudaEventBlockingSync</a>: Specifies that event should use blocking synchronization. A host thread that uses <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1g08241bcf5c5cb686b1882a8492f1e2d9" title="Waits for an event to complete." shape="rect">cudaEventSynchronize()</a> to wait on an event created with this flag will block until the event actually completes.
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ga5d3eff7c3623e2be533968d9cc1ee7e" shape="rect">cudaEventDisableTiming</a>: Specifies that the created event does not need to record timing data. Events created with this flag specified and the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g26509a522be9d449aa7c8c279612452d" shape="rect">cudaEventBlockingSync</a> flag not specified will provide the best performance when used with <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g80c62c379f0c3ed8afe31fd0a31ad8a2" title="Make a compute stream wait on an event." shape="rect">cudaStreamWaitEvent()</a> and <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1gf8e4ddb569b1da032c060f0c54da698f" title="Queries an event's status." shape="rect">cudaEventQuery()</a>.
</p>
</li>
</ul>
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1g320ab51604f3a7a082795202e7eaf774" title="Creates an event object." shape="rect">cudaEventCreate ( C API)</a>, <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1gd5a65651969743246344618073717406" title="Creates an event object with the specified flags." shape="rect">cudaEventCreateWithFlags</a>, <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1ge31b1b1558db52579c9e23c5782af93e" title="Records an event." shape="rect">cudaEventRecord</a>, <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1gf8e4ddb569b1da032c060f0c54da698f" title="Queries an event's status." shape="rect">cudaEventQuery</a>, <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1g08241bcf5c5cb686b1882a8492f1e2d9" title="Waits for an event to complete." shape="rect">cudaEventSynchronize</a>, <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1gff983c870090fcdeec2e948659375079" title="Destroys an event object." shape="rect">cudaEventDestroy</a>, <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1g14c387cc57ce2e328f6669854e6020a5" title="Computes the elapsed time between events." shape="rect">cudaEventElapsedTime</a>, <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g80c62c379f0c3ed8afe31fd0a31ad8a2" title="Make a compute stream wait on an event." shape="rect">cudaStreamWaitEvent</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g0b85e087210b47056cb6fc03a0e264e8" id="group__CUDART__HIGHLEVEL_1g0b85e087210b47056cb6fc03a0e264e8" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaFuncGetAttributes ( <a href="structcudaFuncAttributes.html#structcudaFuncAttributes" title="" shape="rect">cudaFuncAttributes</a>*<span> </span><span class="keyword keyword apiItemName">attr</span>, T*<span> </span><span class="keyword keyword apiItemName">entry</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Find out attributes for a given function </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">attr</span></tt></dt>
<dd>- Return pointer to function's attributes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">entry</span></tt></dt>
<dd>- Function to get attributes of</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038ce7993a88ecf2c57b8102d55d997a18c" shape="rect">cudaErrorInitializationError</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038b6af535e7e53d3f21e2437e8977b8c2e" shape="rect">cudaErrorInvalidDeviceFunction</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>This function obtains the attributes of a function specified via <tt class="ph tt code">entry</tt>. The parameter <tt class="ph tt code">entry</tt> must be a pointer to a function that executes on the device. The parameter specified by <tt class="ph tt code">entry</tt> must be declared as a <tt class="ph tt code">__global__</tt> function. The fetched attributes are placed in <tt class="ph tt code">attr</tt>. If the specified function does not exist, then <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038b6af535e7e53d3f21e2437e8977b8c2e" shape="rect">cudaErrorInvalidDeviceFunction</a> is returned.
</p>
<p class="p">Note that some function attributes such as <a class="xref" href="structcudaFuncAttributes.html#structcudaFuncAttributes_1b8350f491105f159ff684f5c59167af0" shape="rect">maxThreadsPerBlock</a> may vary based on the device that is currently being used.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge0969184de8a5c2d809aa8d7d2425484" title="[C++ API] Sets the preferred cache configuration for a device function" shape="rect">cudaFuncSetCacheConfig ( C++ API)</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g2c1ba377d147198dcc0b631f0193eddc" title="Find out attributes for a given function." shape="rect">cudaFuncGetAttributes ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf9f5de511075f30c1bf97ea4306e9728" title="[C++ API] Launches a device function" shape="rect">cudaLaunch ( C++ API)</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gb9574eae787e2c3c91f4954542b17515" title="Converts a double argument to be executed on a device." shape="rect">cudaSetDoubleForDevice</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g857c928b6e8a9e4c4c2ec4d4cc5c4063" title="Converts a double argument after execution on a device." shape="rect">cudaSetDoubleForHost</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0ffbffed226005960c39688493c94c84" title="[C++ API] Configure a device launch" shape="rect">cudaSetupArgument ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1ge0969184de8a5c2d809aa8d7d2425484" id="group__CUDART__HIGHLEVEL_1ge0969184de8a5c2d809aa8d7d2425484" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaFuncSetCacheConfig ( T*<span> </span><span class="keyword keyword apiItemName">func</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" title="" shape="rect">cudaFuncCache</a><span> </span><span class="keyword keyword apiItemName">cacheConfig</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Sets the preferred cache configuration for a device function </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">func</span></tt></dt>
<dd>- device function pointer </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">cacheConfig</span></tt></dt>
<dd>- Requested cache configuration</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038ce7993a88ecf2c57b8102d55d997a18c" shape="rect">cudaErrorInitializationError</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038b6af535e7e53d3f21e2437e8977b8c2e" shape="rect">cudaErrorInvalidDeviceFunction</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>On devices where the L1 cache and shared memory use the same hardware resources, this sets through <tt class="ph tt code">cacheConfig</tt> the preferred cache configuration for the function specified via <tt class="ph tt code">func</tt>. This is only a preference. The runtime will use the requested configuration if possible, but it is free to choose a different
configuration if required to execute <tt class="ph tt code">func</tt>.
</p>
<p class="p"><tt class="ph tt code">func</tt> must be a pointer to a function that executes on the device. The parameter specified by <tt class="ph tt code">func</tt> must be declared as a <tt class="ph tt code">__global__</tt> function. If the specified function does not exist, then <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038b6af535e7e53d3f21e2437e8977b8c2e" shape="rect">cudaErrorInvalidDeviceFunction</a> is returned.
</p>
<p class="p">This setting does nothing on devices where the size of the L1 cache and shared memory are fixed.</p>
<p class="p">Launching a kernel with a different preference than the most recent preference setting may insert a device-side synchronization
point.
</p>
<p class="p">The supported cache configurations are:
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b3b4b8c65376ce1ca107be413e15981bc" shape="rect">cudaFuncCachePreferNone</a>: no preference for shared memory or L1 (default)
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b84725d25c531f9bafc61ae329afe5b2b" shape="rect">cudaFuncCachePreferShared</a>: prefer larger shared memory and smaller L1 cache
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggb980f35ed69ee7991704de29a13de49b8ecb48ccbc2230c81528a2c7c695100e" shape="rect">cudaFuncCachePreferL1</a>: prefer larger L1 cache and smaller shared memory
</p>
</li>
</ul>
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g4f35d04be20a41c5df96613a748eecc1" title="Sets the preferred cache configuration for a device function." shape="rect">cudaFuncSetCacheConfig ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0b85e087210b47056cb6fc03a0e264e8" title="[C++ API] Find out attributes for a given function" shape="rect">cudaFuncGetAttributes ( C++ API)</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gf4f3215d06b6d90849a3d977f9440002" title="Launches a device function." shape="rect">cudaLaunch ( C API)</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gb9574eae787e2c3c91f4954542b17515" title="Converts a double argument to be executed on a device." shape="rect">cudaSetDoubleForDevice</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g857c928b6e8a9e4c4c2ec4d4cc5c4063" title="Converts a double argument after execution on a device." shape="rect">cudaSetDoubleForHost</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0ffbffed226005960c39688493c94c84" title="[C++ API] Configure a device launch" shape="rect">cudaSetupArgument ( C++ API)</a>, <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1g7a82ef85e4f7e0cff0a84b2f7f6bc63a" title="Returns the preferred cache configuration for the current device." shape="rect">cudaThreadGetCacheConfig</a>, <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1g27d0f538b3018142bf04deae7f02c49e" title="Sets the preferred cache configuration for the current device." shape="rect">cudaThreadSetCacheConfig</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g5ca79fbb1f49f7fb8e45d768418c10f7" id="group__CUDART__HIGHLEVEL_1g5ca79fbb1f49f7fb8e45d768418c10f7" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaGetSymbolAddress ( void**<span> </span><span class="keyword keyword apiItemName">devPtr</span>, const T&<span> </span><span class="keyword keyword apiItemName">symbol</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Finds the address associated with a CUDA symbol </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">devPtr</span></tt></dt>
<dd>- Return device pointer associated with symbol </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">symbol</span></tt></dt>
<dd>- Device symbol reference</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003801a4a97f3060ec714ffa9dd650b9213a" shape="rect">cudaErrorInvalidSymbol</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Returns in <tt class="ph tt code">*devPtr</tt> the address of symbol <tt class="ph tt code">symbol</tt> on the device. <tt class="ph tt code">symbol</tt> can either be a variable that resides in global or constant memory space. If <tt class="ph tt code">symbol</tt> cannot be found, or if <tt class="ph tt code">symbol</tt> is not declared in the global or constant memory space, <tt class="ph tt code">*devPtr</tt> is unchanged and the error <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003801a4a97f3060ec714ffa9dd650b9213a" shape="rect">cudaErrorInvalidSymbol</a> is returned.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g1b2a5ca2b220e77deb6a777bf3f75a65" title="Finds the address associated with a CUDA symbol." shape="rect">cudaGetSymbolAddress ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g9b568e473b813e84aba99c44e6d57a90" title="[C++ API] Finds the size of the object associated with a CUDA symbol" shape="rect">cudaGetSymbolSize ( C++ API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g9b568e473b813e84aba99c44e6d57a90" id="group__CUDART__HIGHLEVEL_1g9b568e473b813e84aba99c44e6d57a90" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaGetSymbolSize ( size_t*<span> </span><span class="keyword keyword apiItemName">size</span>, const T&<span> </span><span class="keyword keyword apiItemName">symbol</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Finds the size of the object associated with a CUDA symbol </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">size</span></tt></dt>
<dd>- Size of object associated with symbol </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">symbol</span></tt></dt>
<dd>- Device symbol reference</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003801a4a97f3060ec714ffa9dd650b9213a" shape="rect">cudaErrorInvalidSymbol</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Returns in <tt class="ph tt code">*size</tt> the size of symbol <tt class="ph tt code">symbol</tt>. <tt class="ph tt code">symbol</tt> must be a variable that resides in global or constant memory space. If <tt class="ph tt code">symbol</tt> cannot be found, or if <tt class="ph tt code">symbol</tt> is not declared in global or constant memory space, <tt class="ph tt code">*size</tt> is unchanged and the error <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003801a4a97f3060ec714ffa9dd650b9213a" shape="rect">cudaErrorInvalidSymbol</a> is returned.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ca79fbb1f49f7fb8e45d768418c10f7" title="[C++ API] Finds the address associated with a CUDA symbol" shape="rect">cudaGetSymbolAddress ( C++ API)</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gc51f29cb96dfd5269bc5b57852fc44a8" title="Finds the size of the object associated with a CUDA symbol." shape="rect">cudaGetSymbolSize ( C API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" id="group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaGetTextureAlignmentOffset ( size_t*<span> </span><span class="keyword keyword apiItemName">offset</span>, const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Get the alignment offset of a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset of texture reference in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture to get offset of</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e4312b7621ebad05ce494249474a7e11" shape="rect">cudaErrorInvalidTexture</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00382e73e27da21d74d0de9eaa8bcd61b527" shape="rect">cudaErrorInvalidTextureBinding</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Returns in <tt class="ph tt code">*offset</tt> the offset that was returned when texture reference <tt class="ph tt code">tex</tt> was bound.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" title="[C++ API] Unbinds a texture" shape="rect">cudaUnbindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g6076c6bf0b1f2e52a36cd51af9d78fb4" title="Get the alignment offset of a texture." shape="rect">cudaGetTextureAlignmentOffset ( C API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1gf9f5de511075f30c1bf97ea4306e9728" id="group__CUDART__HIGHLEVEL_1gf9f5de511075f30c1bf97ea4306e9728" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaLaunch ( T*<span> </span><span class="keyword keyword apiItemName">func</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Launches a device function </div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038b6af535e7e53d3f21e2437e8977b8c2e" shape="rect">cudaErrorInvalidDeviceFunction</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038d3934977826b2e1488dfeb7e0614e776" shape="rect">cudaErrorInvalidConfiguration</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038099def426efea2b2366d8d7ad09f974a" shape="rect">cudaErrorLaunchFailure</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00384ea7f1214c348f64f565ca860933e5a5" shape="rect">cudaErrorLaunchTimeout</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038dfddff5cba4a975a67b298ee0752f714" shape="rect">cudaErrorLaunchOutOfResources</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038fdab7b31b891f328808866b6a933eb0d" shape="rect">cudaErrorSharedObjectSymbolNotFound</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383be0ba00f56924404620f89b7d405362" shape="rect">cudaErrorSharedObjectInitFailed</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Launches the function <tt class="ph tt code">entry</tt> on the device. The parameter <tt class="ph tt code">entry</tt> must be a function that executes on the device. The parameter specified by <tt class="ph tt code">entry</tt> must be declared as a <tt class="ph tt code">__global__</tt> function. <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf9f5de511075f30c1bf97ea4306e9728" title="[C++ API] Launches a device function" shape="rect">cudaLaunch()</a> must be preceded by a call to <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall()</a> since it pops the data that was pushed by <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall()</a> from the execution stack.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge0969184de8a5c2d809aa8d7d2425484" title="[C++ API] Sets the preferred cache configuration for a device function" shape="rect">cudaFuncSetCacheConfig ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0b85e087210b47056cb6fc03a0e264e8" title="[C++ API] Find out attributes for a given function" shape="rect">cudaFuncGetAttributes ( C++ API)</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gf4f3215d06b6d90849a3d977f9440002" title="Launches a device function." shape="rect">cudaLaunch ( C API)</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gb9574eae787e2c3c91f4954542b17515" title="Converts a double argument to be executed on a device." shape="rect">cudaSetDoubleForDevice</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g857c928b6e8a9e4c4c2ec4d4cc5c4063" title="Converts a double argument after execution on a device." shape="rect">cudaSetDoubleForHost</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0ffbffed226005960c39688493c94c84" title="[C++ API] Configure a device launch" shape="rect">cudaSetupArgument ( C++ API)</a>, <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1g7a82ef85e4f7e0cff0a84b2f7f6bc63a" title="Returns the preferred cache configuration for the current device." shape="rect">cudaThreadGetCacheConfig</a>, <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1g27d0f538b3018142bf04deae7f02c49e" title="Sets the preferred cache configuration for the current device." shape="rect">cudaThreadSetCacheConfig</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1ge439496de696b166ba457dab5dd4f356" id="group__CUDART__HIGHLEVEL_1ge439496de696b166ba457dab5dd4f356" shape="rect">
<!-- --></a><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaMallocHost ( void**<span> </span><span class="keyword keyword apiItemName">ptr</span>, size_t<span> </span><span class="keyword keyword apiItemName">size</span>, unsigned int <span> </span><span class="keyword keyword apiItemName">flags</span> ) </span></dt>
<dd class="description">
<div class="section">[C++ API] Allocates page-locked memory on the host </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">ptr</span></tt></dt>
<dd>- Device pointer to allocated memory </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">size</span></tt></dt>
<dd>- Requested allocation size in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">flags</span></tt></dt>
<dd>- Requested properties of allocated memory</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038f210f50ae7f17f655e0504929606add9" shape="rect">cudaErrorMemoryAllocation</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Allocates <tt class="ph tt code">size</tt> bytes of host memory that is page-locked and accessible to the device. The driver tracks the virtual memory ranges allocated
with this function and automatically accelerates calls to functions such as <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g48efa06b81cc031b2aa6fdc2e9930741" title="Copies data between host and device." shape="rect">cudaMemcpy()</a>. Since the memory can be accessed directly by the device, it can be read or written with much higher bandwidth than pageable
memory obtained with functions such as malloc(). Allocating excessive amounts of pinned memory may degrade system performance,
since it reduces the amount of memory available to the system for paging. As a result, this function is best used sparingly
to allocate staging areas for data exchange between host and device.
</p>
<p class="p">The <tt class="ph tt code">flags</tt> parameter enables different options to be specified that affect the allocation, as follows.
<ul class="ul">
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1e00f7734325eb38d75f3ffeae6acac8" shape="rect">cudaHostAllocDefault</a>: This flag's value is defined to be 0.
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gc46ce76be41cf79774331cc8cfceb52b" shape="rect">cudaHostAllocPortable</a>: The memory returned by this call will be considered as pinned memory by all CUDA contexts, not just the one that performed
the allocation.
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" shape="rect">cudaHostAllocMapped</a>: Maps the allocation into the CUDA address space. The device pointer to the memory may be obtained by calling <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1ga475419a9b21a66036029d5001ea908c" title="Passes back device pointer of mapped host memory allocated by cudaHostAlloc or registered by cudaHostRegister." shape="rect">cudaHostGetDevicePointer()</a>.
</p>
</li>
<li class="li">
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g3a7db37d02ce0b2350067ab639ef321c" shape="rect">cudaHostAllocWriteCombined</a>: Allocates the memory as write-combined (WC). WC memory can be transferred across the PCI Express bus more quickly on some
system configurations, but cannot be read efficiently by most CPUs. WC memory is a good option for buffers that will be written
by the CPU and read by the device via mapped pinned memory or host->device transfers.
</p>
</li>
</ul>
</p>
<p class="p">All of these flags are orthogonal to one another: a developer may allocate memory that is portable, mapped and/or write-combined
with no restrictions.
</p>
<p class="p"><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> must have been called with the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g3762be9cccdd809a4ca128354fd134b0" shape="rect">cudaDeviceMapHost</a> flag in order for the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" shape="rect">cudaHostAllocMapped</a> flag to have any effect.
</p>
<p class="p">The <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" shape="rect">cudaHostAllocMapped</a> flag may be specified on CUDA contexts for devices that do not support mapped pinned memory. The failure is deferred to <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1ga475419a9b21a66036029d5001ea908c" title="Passes back device pointer of mapped host memory allocated by cudaHostAlloc or registered by cudaHostRegister." shape="rect">cudaHostGetDevicePointer()</a> because the memory may be mapped into other CUDA contexts via the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gc46ce76be41cf79774331cc8cfceb52b" shape="rect">cudaHostAllocPortable</a> flag.
</p>
<p class="p">Memory allocated by this function must be freed with <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gedaeb2708ad3f74d5b417ee1874ec84a" title="Frees page-locked memory." shape="rect">cudaFreeHost()</a>.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g18074e885b4d89f5a0fe1beab589e0c8" title="Sets flags to be used for device executions." shape="rect">cudaSetDeviceFlags</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g9f93d9600f4504e0d637ceb43c91ebad" title="Allocates page-locked memory on the host." shape="rect">cudaMallocHost ( C API)</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gedaeb2708ad3f74d5b417ee1874ec84a" title="Frees page-locked memory." shape="rect">cudaFreeHost</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g15a3871f15f8c38f5b7190946845758c" title="Allocates page-locked memory on the host." shape="rect">cudaHostAlloc</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" id="group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaMallocManaged ( T**<span> </span><span class="keyword keyword apiItemName">devPtr</span>, size_t<span> </span><span class="keyword keyword apiItemName">size</span>, unsigned int <span> </span><span class="keyword keyword apiItemName">flags</span> = <span class="ph ph apiData">cudaMemAttachGlobal</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">Allocates memory that will be automatically managed by the Unified Memory system. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">devPtr</span></tt></dt>
<dd>- Pointer to allocated device memory </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">size</span></tt></dt>
<dd>- Requested allocation size in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">flags</span></tt></dt>
<dd>- Must be either <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a> or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">cudaMemAttachHost</a> (defaults to <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a>)
</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038f210f50ae7f17f655e0504929606add9" shape="rect">cudaErrorMemoryAllocation</a><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038d846fd9f2e8ba5e2fb4f1695b7ab6164" shape="rect">cudaErrorNotSupported</a><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Allocates <tt class="ph tt code">size</tt> bytes of managed memory on the device and returns in <tt class="ph tt code">*devPtr</tt> a pointer to the allocated memory. If the device doesn't support allocating managed memory, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038d846fd9f2e8ba5e2fb4f1695b7ab6164" shape="rect">cudaErrorNotSupported</a> is returned. Support for managed memory can be queried using the device attribute <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg49e2f8c2c0bd6fe264f2fc970912e5cd5467985f87821a03625ab62e72195ff8" shape="rect">cudaDevAttrManagedMemory</a>. The allocated memory is suitably aligned for any kind of variable. The memory is not cleared. If <tt class="ph tt code">size</tt> is 0, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" title="Allocates memory that will be automatically managed by the Unified Memory system." shape="rect">cudaMallocManaged</a> returns <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>. The pointer is valid on the CPU and on all GPUs in the system that support managed memory. All accesses to this pointer
must obey the Unified Memory programming model.
</p>
<p class="p"><tt class="ph tt code">flags</tt> specifies the default stream association for this allocation. <tt class="ph tt code">flags</tt> must be one of <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a> or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">cudaMemAttachHost</a>. The default value for <tt class="ph tt code">flags</tt> is <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a>. If <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a> is specified, then this memory is accessible from any stream on any device. If <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">cudaMemAttachHost</a> is specified, then the allocation is created with initial visibility restricted to host access only; an explicit call to
<a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gebe68658a891edc398791a436a8e1d7c" title="Attach memory to a stream asynchronously." shape="rect">cudaStreamAttachMemAsync</a> will be required to enable access on the device.
</p>
<p class="p">If the association is later changed via <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gebe68658a891edc398791a436a8e1d7c" title="Attach memory to a stream asynchronously." shape="rect">cudaStreamAttachMemAsync</a> to a single stream, the default association, as specifed during <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" title="Allocates memory that will be automatically managed by the Unified Memory system." shape="rect">cudaMallocManaged</a>, is restored when that stream is destroyed. For __managed__ variables, the default association is always <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a>. Note that destroying a stream is an asynchronous operation, and as a result, the change to default association won't happen
until all work in the stream has completed.
</p>
<p class="p">Memory allocated with <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" title="Allocates memory that will be automatically managed by the Unified Memory system." shape="rect">cudaMallocManaged</a> should be released with <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g02b08ab28cfc28c37976556044fb5335" title="Frees memory on the device." shape="rect">cudaFree</a>.
</p>
<p class="p">On a multi-GPU system with peer-to-peer support, where multiple GPUs support managed memory, the physical storage is created
on the GPU which is active at the time <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" title="Allocates memory that will be automatically managed by the Unified Memory system." shape="rect">cudaMallocManaged</a> is called. All other GPUs will reference the data at reduced bandwidth via peer mappings over the PCIe bus. The Unified Memory
management system does not migrate memory between GPUs.
</p>
<p class="p">On a multi-GPU system where multiple GPUs support managed memory, but not all pairs of such GPUs have peer-to-peer support
between them, the physical storage is created in 'zero-copy' or system memory. All GPUs will reference the data at reduced
bandwidth over the PCIe bus. In these circumstances, use of the environment variable, CUDA_VISIBLE_DEVICES, is recommended
to restrict CUDA to only use those GPUs that have peer-to-peer support. Alternatively, users can also set CUDA_MANAGED_FORCE_DEVICE_ALLOC
to a non-zero value to force the driver to always use device memory for physical storage. When this environment variable is
set to a non-zero value, all devices used in that process that support managed memory have to be peer-to-peer compatible with
each other. The error <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038938c6e8b96ecde62e3ab5137156f739a" shape="rect">cudaErrorInvalidDevice</a> will be returned if a device that supports managed memory is used and it is not peer-to-peer compatible with any of the other
managed memory supporting devices that were previously used in that process, even if <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1gdcc2c6f914eb9461565b12648faa5e28" title="Destroy all allocations and reset all state on the current device in the current process." shape="rect">cudaDeviceReset</a> has been called on those devices. These environment variables are described in the CUDA programming guide under the "CUDA
environment variables" section.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g80d689bc903792f906e49be4a0b6d8db" title="Allocates pitched memory on the device." shape="rect">cudaMallocPitch</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g02b08ab28cfc28c37976556044fb5335" title="Frees memory on the device." shape="rect">cudaFree</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g6c5308ef1b088989cbf8a7500918584e" title="Allocate an array on the device." shape="rect">cudaMallocArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gfca922b03993e6cb33954cf50776987b" title="Frees an array on the device." shape="rect">cudaFreeArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g04a7553c90322aef32f8544d5c356a10" title="Allocates logical 1D, 2D, or 3D memory objects on the device." shape="rect">cudaMalloc3D</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g99ad4e156b725f4ad908e52cf09d5ad1" title="Allocate an array on the device." shape="rect">cudaMalloc3DArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g9f93d9600f4504e0d637ceb43c91ebad" title="Allocates page-locked memory on the host." shape="rect">cudaMallocHost ( C API)</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gedaeb2708ad3f74d5b417ee1874ec84a" title="Frees page-locked memory." shape="rect">cudaFreeHost</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g15a3871f15f8c38f5b7190946845758c" title="Allocates page-locked memory on the host." shape="rect">cudaHostAlloc</a>, <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g1b092b57223ac999485f351c0e0f8ec8" title="Returns information about the device." shape="rect">cudaDeviceGetAttribute</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gebe68658a891edc398791a436a8e1d7c" title="Attach memory to a stream asynchronously." shape="rect">cudaStreamAttachMemAsync</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g6a9b39c2d139205e60c107c8f1802775" id="group__CUDART__HIGHLEVEL_1g6a9b39c2d139205e60c107c8f1802775" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaMemcpyFromSymbol ( void*<span> </span><span class="keyword keyword apiItemName">dst</span>, const T&<span> </span><span class="keyword keyword apiItemName">symbol</span>, size_t<span> </span><span class="keyword keyword apiItemName">count</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> = <span class="ph ph apiData">0</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" title="" shape="rect">cudaMemcpyKind</a><span> </span><span class="keyword keyword apiItemName">kind</span> = <span class="ph ph apiData">cudaMemcpyDeviceToHost</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Copies data from the given symbol on the device </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">dst</span></tt></dt>
<dd>- Destination memory address </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">symbol</span></tt></dt>
<dd>- Device symbol reference </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">count</span></tt></dt>
<dd>- Size in bytes to copy </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset from start of symbol in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">kind</span></tt></dt>
<dd>- Type of transfer</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003801a4a97f3060ec714ffa9dd650b9213a" shape="rect">cudaErrorInvalidSymbol</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003872ce39cee8ef48a83b0191b2e33d2630" shape="rect">cudaErrorInvalidMemcpyDirection</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Copies <tt class="ph tt code">count</tt> bytes from the memory area <tt class="ph tt code">offset</tt> bytes from the start of symbol <tt class="ph tt code">symbol</tt> to the memory area pointed to by <tt class="ph tt code">dst</tt>. The memory areas may not overlap. <tt class="ph tt code">symbol</tt> is a variable that resides in global or constant memory space. <tt class="ph tt code">kind</tt> can be either <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b5653197602d3455a530db5a7edb1a253" shape="rect">cudaMemcpyDeviceToHost</a> or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b783338534304281650c6cb1363f5a00a" shape="rect">cudaMemcpyDeviceToDevice</a>.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><ul class="ul">
<li class="li">
<p class="p">Note that this function may also return error codes from previous, asynchronous launches. </p>
</li>
<li class="li">
<p class="p">This function exhibits <a class="xref xmlonly" href="api-sync-behavior.html#api-sync-behavior__memcpy-sync" shape="rect">synchronous</a> behavior for most use cases.
</p>
</li>
<li class="li">
<p class="p">Use of a string naming a variable as the <tt class="ph tt code">symbol</tt> paramater was deprecated in CUDA 4.1 and removed in CUDA 5.0.
</p>
</li>
</ul>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g48efa06b81cc031b2aa6fdc2e9930741" title="Copies data between host and device." shape="rect">cudaMemcpy</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g17f3a55e8c9aef5f90b67cdf22851375" title="Copies data between host and device." shape="rect">cudaMemcpy2D</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g8bb7cc359d74e394138d980e340ccbe4" title="Copies data between host and device." shape="rect">cudaMemcpyToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gc7194df1302ec7459416218b4ea04034" title="Copies data between host and device." shape="rect">cudaMemcpy2DToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g1d8c74f2a06e8f5f34fc5e455d88a04c" title="Copies data between host and device." shape="rect">cudaMemcpyFromArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g2d9dc2f6bdd394417ddae8972f29f82a" title="Copies data between host and device." shape="rect">cudaMemcpy2DFromArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g455873a8bc760eb6f0faee1cb57ec204" title="Copies data between host and device." shape="rect">cudaMemcpyArrayToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g42ffb085a69543f835f074128e6aa1aa" title="Copies data between host and device." shape="rect">cudaMemcpy2DArrayToArray</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0c15b63c7b065fda8998713831edcbc7" title="[C++ API] Copies data to the given symbol on the device" shape="rect">cudaMemcpyToSymbol</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gf2810a94ec08fe3c7ff9d93a33af7255" title="Copies data between host and device." shape="rect">cudaMemcpyAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g7f182f1a8b8750c7fa9e18aeb280d31c" title="Copies data between host and device." shape="rect">cudaMemcpy2DAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gbf276f587fe8d7af71c9b184e3660866" title="Copies data between host and device." shape="rect">cudaMemcpyToArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g570be5f0c9c997125e77e26da35e2ec7" title="Copies data between host and device." shape="rect">cudaMemcpy2DToArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gf8159b9bf3cc5adb607a6e207159d61a" title="Copies data between host and device." shape="rect">cudaMemcpyFromArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g2a1ed39c8ebdc41c3dd5e92901e0f754" title="Copies data between host and device." shape="rect">cudaMemcpy2DFromArrayAsync</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf04a6abff5155d11b12c35fe14a98280" title="[C++ API] Copies data to the given symbol on the device" shape="rect">cudaMemcpyToSymbolAsync</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge8a47aa428b24d05e3a1bccff673a7c9" title="[C++ API] Copies data from the given symbol on the device" shape="rect">cudaMemcpyFromSymbolAsync</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1ge8a47aa428b24d05e3a1bccff673a7c9" id="group__CUDART__HIGHLEVEL_1ge8a47aa428b24d05e3a1bccff673a7c9" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaMemcpyFromSymbolAsync ( void*<span> </span><span class="keyword keyword apiItemName">dst</span>, const T&<span> </span><span class="keyword keyword apiItemName">symbol</span>, size_t<span> </span><span class="keyword keyword apiItemName">count</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> = <span class="ph ph apiData">0</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" title="" shape="rect">cudaMemcpyKind</a><span> </span><span class="keyword keyword apiItemName">kind</span> = <span class="ph ph apiData">cudaMemcpyDeviceToHost</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" title="" shape="rect">cudaStream_t</a><span> </span><span class="keyword keyword apiItemName">stream</span> = <span class="ph ph apiData">0</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Copies data from the given symbol on the device </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">dst</span></tt></dt>
<dd>- Destination memory address </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">symbol</span></tt></dt>
<dd>- Device symbol reference </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">count</span></tt></dt>
<dd>- Size in bytes to copy </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset from start of symbol in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">kind</span></tt></dt>
<dd>- Type of transfer </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">stream</span></tt></dt>
<dd>- Stream identifier</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003801a4a97f3060ec714ffa9dd650b9213a" shape="rect">cudaErrorInvalidSymbol</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003872ce39cee8ef48a83b0191b2e33d2630" shape="rect">cudaErrorInvalidMemcpyDirection</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Copies <tt class="ph tt code">count</tt> bytes from the memory area <tt class="ph tt code">offset</tt> bytes from the start of symbol <tt class="ph tt code">symbol</tt> to the memory area pointed to by <tt class="ph tt code">dst</tt>. The memory areas may not overlap. <tt class="ph tt code">symbol</tt> is a variable that resides in global or constant memory space. <tt class="ph tt code">kind</tt> can be either <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b5653197602d3455a530db5a7edb1a253" shape="rect">cudaMemcpyDeviceToHost</a> or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b783338534304281650c6cb1363f5a00a" shape="rect">cudaMemcpyDeviceToDevice</a>.
</p>
<p class="p"><a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g44e13909cc759d6af69dad07d9cdf25d" title="Copies data from the given symbol on the device." shape="rect">cudaMemcpyFromSymbolAsync()</a> is asynchronous with respect to the host, so the call may return before the copy is complete. The copy can optionally be
associated to a stream by passing a non-zero <tt class="ph tt code">stream</tt> argument. If <tt class="ph tt code">kind</tt> is <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b5653197602d3455a530db5a7edb1a253" shape="rect">cudaMemcpyDeviceToHost</a> and <tt class="ph tt code">stream</tt> is non-zero, the copy may overlap with operations in other streams.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><ul class="ul">
<li class="li">
<p class="p">Note that this function may also return error codes from previous, asynchronous launches. </p>
</li>
<li class="li">
<p class="p">This function exhibits <a class="xref xmlonly" href="api-sync-behavior.html#api-sync-behavior__memcpy-async" shape="rect">asynchronous</a> behavior for most use cases.
</p>
</li>
<li class="li">
<p class="p">Use of a string naming a variable as the <tt class="ph tt code">symbol</tt> paramater was deprecated in CUDA 4.1 and removed in CUDA 5.0.
</p>
</li>
</ul>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g48efa06b81cc031b2aa6fdc2e9930741" title="Copies data between host and device." shape="rect">cudaMemcpy</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g17f3a55e8c9aef5f90b67cdf22851375" title="Copies data between host and device." shape="rect">cudaMemcpy2D</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g8bb7cc359d74e394138d980e340ccbe4" title="Copies data between host and device." shape="rect">cudaMemcpyToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gc7194df1302ec7459416218b4ea04034" title="Copies data between host and device." shape="rect">cudaMemcpy2DToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g1d8c74f2a06e8f5f34fc5e455d88a04c" title="Copies data between host and device." shape="rect">cudaMemcpyFromArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g2d9dc2f6bdd394417ddae8972f29f82a" title="Copies data between host and device." shape="rect">cudaMemcpy2DFromArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g455873a8bc760eb6f0faee1cb57ec204" title="Copies data between host and device." shape="rect">cudaMemcpyArrayToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g42ffb085a69543f835f074128e6aa1aa" title="Copies data between host and device." shape="rect">cudaMemcpy2DArrayToArray</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0c15b63c7b065fda8998713831edcbc7" title="[C++ API] Copies data to the given symbol on the device" shape="rect">cudaMemcpyToSymbol</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g6a9b39c2d139205e60c107c8f1802775" title="[C++ API] Copies data from the given symbol on the device" shape="rect">cudaMemcpyFromSymbol</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gf2810a94ec08fe3c7ff9d93a33af7255" title="Copies data between host and device." shape="rect">cudaMemcpyAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g7f182f1a8b8750c7fa9e18aeb280d31c" title="Copies data between host and device." shape="rect">cudaMemcpy2DAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gbf276f587fe8d7af71c9b184e3660866" title="Copies data between host and device." shape="rect">cudaMemcpyToArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g570be5f0c9c997125e77e26da35e2ec7" title="Copies data between host and device." shape="rect">cudaMemcpy2DToArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gf8159b9bf3cc5adb607a6e207159d61a" title="Copies data between host and device." shape="rect">cudaMemcpyFromArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g2a1ed39c8ebdc41c3dd5e92901e0f754" title="Copies data between host and device." shape="rect">cudaMemcpy2DFromArrayAsync</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf04a6abff5155d11b12c35fe14a98280" title="[C++ API] Copies data to the given symbol on the device" shape="rect">cudaMemcpyToSymbolAsync</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g0c15b63c7b065fda8998713831edcbc7" id="group__CUDART__HIGHLEVEL_1g0c15b63c7b065fda8998713831edcbc7" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaMemcpyToSymbol ( const T&<span> </span><span class="keyword keyword apiItemName">symbol</span>, const void*<span> </span><span class="keyword keyword apiItemName">src</span>, size_t<span> </span><span class="keyword keyword apiItemName">count</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> = <span class="ph ph apiData">0</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" title="" shape="rect">cudaMemcpyKind</a><span> </span><span class="keyword keyword apiItemName">kind</span> = <span class="ph ph apiData">cudaMemcpyHostToDevice</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Copies data to the given symbol on the device </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">symbol</span></tt></dt>
<dd>- Device symbol reference </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">src</span></tt></dt>
<dd>- Source memory address </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">count</span></tt></dt>
<dd>- Size in bytes to copy </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset from start of symbol in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">kind</span></tt></dt>
<dd>- Type of transfer</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003801a4a97f3060ec714ffa9dd650b9213a" shape="rect">cudaErrorInvalidSymbol</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003872ce39cee8ef48a83b0191b2e33d2630" shape="rect">cudaErrorInvalidMemcpyDirection</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Copies <tt class="ph tt code">count</tt> bytes from the memory area pointed to by <tt class="ph tt code">src</tt> to the memory area <tt class="ph tt code">offset</tt> bytes from the start of symbol <tt class="ph tt code">symbol</tt>. The memory areas may not overlap. <tt class="ph tt code">symbol</tt> is a variable that resides in global or constant memory space. <tt class="ph tt code">kind</tt> can be either <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b1a03d03a676ea8ec51b9b1e193617568" shape="rect">cudaMemcpyHostToDevice</a> or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b783338534304281650c6cb1363f5a00a" shape="rect">cudaMemcpyDeviceToDevice</a>.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><ul class="ul">
<li class="li">
<p class="p">Note that this function may also return error codes from previous, asynchronous launches. </p>
</li>
<li class="li">
<p class="p">This function exhibits <a class="xref xmlonly" href="api-sync-behavior.html#api-sync-behavior__memcpy-sync" shape="rect">synchronous</a> behavior for most use cases.
</p>
</li>
<li class="li">
<p class="p">Use of a string naming a variable as the <tt class="ph tt code">symbol</tt> paramater was deprecated in CUDA 4.1 and removed in CUDA 5.0.
</p>
</li>
</ul>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g48efa06b81cc031b2aa6fdc2e9930741" title="Copies data between host and device." shape="rect">cudaMemcpy</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g17f3a55e8c9aef5f90b67cdf22851375" title="Copies data between host and device." shape="rect">cudaMemcpy2D</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g8bb7cc359d74e394138d980e340ccbe4" title="Copies data between host and device." shape="rect">cudaMemcpyToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gc7194df1302ec7459416218b4ea04034" title="Copies data between host and device." shape="rect">cudaMemcpy2DToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g1d8c74f2a06e8f5f34fc5e455d88a04c" title="Copies data between host and device." shape="rect">cudaMemcpyFromArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g2d9dc2f6bdd394417ddae8972f29f82a" title="Copies data between host and device." shape="rect">cudaMemcpy2DFromArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g455873a8bc760eb6f0faee1cb57ec204" title="Copies data between host and device." shape="rect">cudaMemcpyArrayToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g42ffb085a69543f835f074128e6aa1aa" title="Copies data between host and device." shape="rect">cudaMemcpy2DArrayToArray</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g6a9b39c2d139205e60c107c8f1802775" title="[C++ API] Copies data from the given symbol on the device" shape="rect">cudaMemcpyFromSymbol</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gf2810a94ec08fe3c7ff9d93a33af7255" title="Copies data between host and device." shape="rect">cudaMemcpyAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g7f182f1a8b8750c7fa9e18aeb280d31c" title="Copies data between host and device." shape="rect">cudaMemcpy2DAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gbf276f587fe8d7af71c9b184e3660866" title="Copies data between host and device." shape="rect">cudaMemcpyToArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g570be5f0c9c997125e77e26da35e2ec7" title="Copies data between host and device." shape="rect">cudaMemcpy2DToArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gf8159b9bf3cc5adb607a6e207159d61a" title="Copies data between host and device." shape="rect">cudaMemcpyFromArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g2a1ed39c8ebdc41c3dd5e92901e0f754" title="Copies data between host and device." shape="rect">cudaMemcpy2DFromArrayAsync</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf04a6abff5155d11b12c35fe14a98280" title="[C++ API] Copies data to the given symbol on the device" shape="rect">cudaMemcpyToSymbolAsync</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge8a47aa428b24d05e3a1bccff673a7c9" title="[C++ API] Copies data from the given symbol on the device" shape="rect">cudaMemcpyFromSymbolAsync</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1gf04a6abff5155d11b12c35fe14a98280" id="group__CUDART__HIGHLEVEL_1gf04a6abff5155d11b12c35fe14a98280" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaMemcpyToSymbolAsync ( const T&<span> </span><span class="keyword keyword apiItemName">symbol</span>, const void*<span> </span><span class="keyword keyword apiItemName">src</span>, size_t<span> </span><span class="keyword keyword apiItemName">count</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> = <span class="ph ph apiData">0</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" title="" shape="rect">cudaMemcpyKind</a><span> </span><span class="keyword keyword apiItemName">kind</span> = <span class="ph ph apiData">cudaMemcpyHostToDevice</span>, <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" title="" shape="rect">cudaStream_t</a><span> </span><span class="keyword keyword apiItemName">stream</span> = <span class="ph ph apiData">0</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Copies data to the given symbol on the device </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">symbol</span></tt></dt>
<dd>- Device symbol reference </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">src</span></tt></dt>
<dd>- Source memory address </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">count</span></tt></dt>
<dd>- Size in bytes to copy </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset from start of symbol in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">kind</span></tt></dt>
<dd>- Type of transfer </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">stream</span></tt></dt>
<dd>- Stream identifier</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003801a4a97f3060ec714ffa9dd650b9213a" shape="rect">cudaErrorInvalidSymbol</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00385fa2f00ab72ab5cf649a0a32351a20bf" shape="rect">cudaErrorInvalidDevicePointer</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e003872ce39cee8ef48a83b0191b2e33d2630" shape="rect">cudaErrorInvalidMemcpyDirection</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Copies <tt class="ph tt code">count</tt> bytes from the memory area pointed to by <tt class="ph tt code">src</tt> to the memory area <tt class="ph tt code">offset</tt> bytes from the start of symbol <tt class="ph tt code">symbol</tt>. The memory areas may not overlap. <tt class="ph tt code">symbol</tt> is a variable that resides in global or constant memory space. <tt class="ph tt code">kind</tt> can be either <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b1a03d03a676ea8ec51b9b1e193617568" shape="rect">cudaMemcpyHostToDevice</a> or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b783338534304281650c6cb1363f5a00a" shape="rect">cudaMemcpyDeviceToDevice</a>.
</p>
<p class="p"><a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g509321f00035f2e40b47c4c5cf372245" title="Copies data to the given symbol on the device." shape="rect">cudaMemcpyToSymbolAsync()</a> is asynchronous with respect to the host, so the call may return before the copy is complete. The copy can optionally be
associated to a stream by passing a non-zero <tt class="ph tt code">stream</tt> argument. If <tt class="ph tt code">kind</tt> is <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg18fa99055ee694244a270e4d5101e95b1a03d03a676ea8ec51b9b1e193617568" shape="rect">cudaMemcpyHostToDevice</a> and <tt class="ph tt code">stream</tt> is non-zero, the copy may overlap with operations in other streams.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><ul class="ul">
<li class="li">
<p class="p">Note that this function may also return error codes from previous, asynchronous launches. </p>
</li>
<li class="li">
<p class="p">This function exhibits <a class="xref xmlonly" href="api-sync-behavior.html#api-sync-behavior__memcpy-async" shape="rect">asynchronous</a> behavior for most use cases.
</p>
</li>
<li class="li">
<p class="p">Use of a string naming a variable as the <tt class="ph tt code">symbol</tt> paramater was deprecated in CUDA 4.1 and removed in CUDA 5.0.
</p>
</li>
</ul>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g48efa06b81cc031b2aa6fdc2e9930741" title="Copies data between host and device." shape="rect">cudaMemcpy</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g17f3a55e8c9aef5f90b67cdf22851375" title="Copies data between host and device." shape="rect">cudaMemcpy2D</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g8bb7cc359d74e394138d980e340ccbe4" title="Copies data between host and device." shape="rect">cudaMemcpyToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gc7194df1302ec7459416218b4ea04034" title="Copies data between host and device." shape="rect">cudaMemcpy2DToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g1d8c74f2a06e8f5f34fc5e455d88a04c" title="Copies data between host and device." shape="rect">cudaMemcpyFromArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g2d9dc2f6bdd394417ddae8972f29f82a" title="Copies data between host and device." shape="rect">cudaMemcpy2DFromArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g455873a8bc760eb6f0faee1cb57ec204" title="Copies data between host and device." shape="rect">cudaMemcpyArrayToArray</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g42ffb085a69543f835f074128e6aa1aa" title="Copies data between host and device." shape="rect">cudaMemcpy2DArrayToArray</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0c15b63c7b065fda8998713831edcbc7" title="[C++ API] Copies data to the given symbol on the device" shape="rect">cudaMemcpyToSymbol</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g6a9b39c2d139205e60c107c8f1802775" title="[C++ API] Copies data from the given symbol on the device" shape="rect">cudaMemcpyFromSymbol</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gf2810a94ec08fe3c7ff9d93a33af7255" title="Copies data between host and device." shape="rect">cudaMemcpyAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g7f182f1a8b8750c7fa9e18aeb280d31c" title="Copies data between host and device." shape="rect">cudaMemcpy2DAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gbf276f587fe8d7af71c9b184e3660866" title="Copies data between host and device." shape="rect">cudaMemcpyToArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g570be5f0c9c997125e77e26da35e2ec7" title="Copies data between host and device." shape="rect">cudaMemcpy2DToArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gf8159b9bf3cc5adb607a6e207159d61a" title="Copies data between host and device." shape="rect">cudaMemcpyFromArrayAsync</a>, <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g2a1ed39c8ebdc41c3dd5e92901e0f754" title="Copies data between host and device." shape="rect">cudaMemcpy2DFromArrayAsync</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge8a47aa428b24d05e3a1bccff673a7c9" title="[C++ API] Copies data from the given symbol on the device" shape="rect">cudaMemcpyFromSymbolAsync</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1gec01149f3a448009f4198fcd810ffc8d" id="group__CUDART__HIGHLEVEL_1gec01149f3a448009f4198fcd810ffc8d" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaOccupancyMaxActiveBlocksPerMultiprocessor ( int*<span> </span><span class="keyword keyword apiItemName">numBlocks</span>, T<span> </span><span class="keyword keyword apiItemName">func</span>, int <span> </span><span class="keyword keyword apiItemName">blockSize</span>, size_t<span> </span><span class="keyword keyword apiItemName">dynamicSMemSize</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">Returns occupancy for a device function. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">numBlocks</span></tt></dt>
<dd>- Returned occupancy </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">func</span></tt></dt>
<dd>- Kernel function for which occupancy is calulated </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">blockSize</span></tt></dt>
<dd>- Block size the kernel is intended to be launched with </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">dynamicSMemSize</span></tt></dt>
<dd>- Per-block dynamic shared memory usage intended, in bytes</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038dfb63bb6ca267fd750bbf85d65f77b01" shape="rect">cudaErrorCudartUnloading</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038ce7993a88ecf2c57b8102d55d997a18c" shape="rect">cudaErrorInitializationError</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038938c6e8b96ecde62e3ab5137156f739a" shape="rect">cudaErrorInvalidDevice</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038b6af535e7e53d3f21e2437e8977b8c2e" shape="rect">cudaErrorInvalidDeviceFunction</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00382e491daacef266c7b3e3c1e140a6133c" shape="rect">cudaErrorUnknown</a>,
</p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Returns in <tt class="ph tt code">*numBlocks</tt> the maximum number of active blocks per streaming multiprocessor for the device function.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gccd34d08d6ae77b0f61beed7afcf66d9" title="Returns grid and block size that achieves maximum potential occupancy for a device function." shape="rect">cudaOccupancyMaxPotentialBlockSize</a></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf69042ce23b8500b972fd74d2ae52bf0" title="Returns grid and block size that achieves maximum potential occupancy for a device function." shape="rect">cudaOccupancyMaxPotentialBlockSizeVariableSMem</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1gccd34d08d6ae77b0f61beed7afcf66d9" id="group__CUDART__HIGHLEVEL_1gccd34d08d6ae77b0f61beed7afcf66d9" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaOccupancyMaxPotentialBlockSize ( int*<span> </span><span class="keyword keyword apiItemName">minGridSize</span>, int*<span> </span><span class="keyword keyword apiItemName">blockSize</span>, T<span> </span><span class="keyword keyword apiItemName">func</span>, size_t<span> </span><span class="keyword keyword apiItemName">dynamicSMemSize</span> = <span class="ph ph apiData">0</span>, int <span> </span><span class="keyword keyword apiItemName">blockSizeLimit</span> = <span class="ph ph apiData">0</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">Returns grid and block size that achieves maximum potential occupancy for a device function. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">minGridSize</span></tt></dt>
<dd>- Returned minimum grid size needed to achieve the best potential occupancy </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">blockSize</span></tt></dt>
<dd>- Returned block size </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">func</span></tt></dt>
<dd>- Device function symbol </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">dynamicSMemSize</span></tt></dt>
<dd>- Per-block dynamic shared memory usage intended, in bytes </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">blockSizeLimit</span></tt></dt>
<dd>- The maximum block size <tt class="ph tt code">func</tt> is designed to work with. 0 means no limit.
</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038dfb63bb6ca267fd750bbf85d65f77b01" shape="rect">cudaErrorCudartUnloading</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038ce7993a88ecf2c57b8102d55d997a18c" shape="rect">cudaErrorInitializationError</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038938c6e8b96ecde62e3ab5137156f739a" shape="rect">cudaErrorInvalidDevice</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038b6af535e7e53d3f21e2437e8977b8c2e" shape="rect">cudaErrorInvalidDeviceFunction</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00382e491daacef266c7b3e3c1e140a6133c" shape="rect">cudaErrorUnknown</a>,
</p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Returns in <tt class="ph tt code">*minGridSize</tt> and <tt class="ph tt code">*blocksize</tt> a suggested grid / block size pair that achieves the best potential occupancy (i.e. the maximum number of active warps with
the smallest number of blocks).
</p>
<p class="p">Use </p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf69042ce23b8500b972fd74d2ae52bf0" title="Returns grid and block size that achieves maximum potential occupancy for a device function." shape="rect">cudaOccupancyMaxPotentialBlockSizeVariableSMem</a> if the amount of per-block dynamic shared memory changes with different block sizes.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gec01149f3a448009f4198fcd810ffc8d" title="Returns occupancy for a device function." shape="rect">cudaOccupancyMaxActiveBlocksPerMultiprocessor</a></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf69042ce23b8500b972fd74d2ae52bf0" title="Returns grid and block size that achieves maximum potential occupancy for a device function." shape="rect">cudaOccupancyMaxPotentialBlockSizeVariableSMem</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1gf69042ce23b8500b972fd74d2ae52bf0" id="group__CUDART__HIGHLEVEL_1gf69042ce23b8500b972fd74d2ae52bf0" shape="rect">
<!-- --></a><p class="template">template < typename UnaryFunction, class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaOccupancyMaxPotentialBlockSizeVariableSMem ( int*<span> </span><span class="keyword keyword apiItemName">minGridSize</span>, int*<span> </span><span class="keyword keyword apiItemName">blockSize</span>, T<span> </span><span class="keyword keyword apiItemName">func</span>, UnaryFunction<span> </span><span class="keyword keyword apiItemName">blockSizeToDynamicSMemSize</span>, int <span> </span><span class="keyword keyword apiItemName">blockSizeLimit</span> = <span class="ph ph apiData">0</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">Returns grid and block size that achieves maximum potential occupancy for a device function. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">minGridSize</span></tt></dt>
<dd>- Returned minimum grid size needed to achieve the best potential occupancy </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">blockSize</span></tt></dt>
<dd>- Returned block size </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">func</span></tt></dt>
<dd>- Device function symbol </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">blockSizeToDynamicSMemSize</span></tt></dt>
<dd>- A unary function / functor that takes block size, and returns the size, in bytes, of dynamic shared memory needed for a
block
</dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">blockSizeLimit</span></tt></dt>
<dd>- The maximum block size <tt class="ph tt code">func</tt> is designed to work with. 0 means no limit.
</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038dfb63bb6ca267fd750bbf85d65f77b01" shape="rect">cudaErrorCudartUnloading</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038ce7993a88ecf2c57b8102d55d997a18c" shape="rect">cudaErrorInitializationError</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038938c6e8b96ecde62e3ab5137156f739a" shape="rect">cudaErrorInvalidDevice</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038b6af535e7e53d3f21e2437e8977b8c2e" shape="rect">cudaErrorInvalidDeviceFunction</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00382e491daacef266c7b3e3c1e140a6133c" shape="rect">cudaErrorUnknown</a>,
</p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Returns in <tt class="ph tt code">*minGridSize</tt> and <tt class="ph tt code">*blocksize</tt> a suggested grid / block size pair that achieves the best potential occupancy (i.e. the maximum number of active warps with
the smallest number of blocks).
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gec01149f3a448009f4198fcd810ffc8d" title="Returns occupancy for a device function." shape="rect">cudaOccupancyMaxActiveBlocksPerMultiprocessor</a></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gccd34d08d6ae77b0f61beed7afcf66d9" title="Returns grid and block size that achieves maximum potential occupancy for a device function." shape="rect">cudaOccupancyMaxPotentialBlockSize</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g0ffbffed226005960c39688493c94c84" id="group__CUDART__HIGHLEVEL_1g0ffbffed226005960c39688493c94c84" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaSetupArgument ( T<span> </span><span class="keyword keyword apiItemName">arg</span>, size_t<span> </span><span class="keyword keyword apiItemName">offset</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Configure a device launch </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">arg</span></tt></dt>
<dd>- Argument to push for a kernel launch </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">offset</span></tt></dt>
<dd>- Offset in argument stack to push new arg</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Pushes <tt class="ph tt code">size</tt> bytes of the argument pointed to by <tt class="ph tt code">arg</tt> at <tt class="ph tt code">offset</tt> bytes from the start of the parameter passing area, which starts at offset 0. The arguments are stored in the top of the
execution stack. <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0ffbffed226005960c39688493c94c84" title="[C++ API] Configure a device launch" shape="rect">cudaSetupArgument()</a> must be preceded by a call to <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall()</a>.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0b85e087210b47056cb6fc03a0e264e8" title="[C++ API] Find out attributes for a given function" shape="rect">cudaFuncGetAttributes ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gf9f5de511075f30c1bf97ea4306e9728" title="[C++ API] Launches a device function" shape="rect">cudaLaunch ( C++ API)</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gb9574eae787e2c3c91f4954542b17515" title="Converts a double argument to be executed on a device." shape="rect">cudaSetDoubleForDevice</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g857c928b6e8a9e4c4c2ec4d4cc5c4063" title="Converts a double argument after execution on a device." shape="rect">cudaSetDoubleForHost</a>, <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gad1ff3ec13bd21524425779542eca8ef" title="Configure a device launch." shape="rect">cudaSetupArgument ( C API)</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1gebe68658a891edc398791a436a8e1d7c" id="group__CUDART__HIGHLEVEL_1gebe68658a891edc398791a436a8e1d7c" shape="rect">
<!-- --></a><p class="template">template < class T ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaStreamAttachMemAsync ( <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" title="" shape="rect">cudaStream_t</a><span> </span><span class="keyword keyword apiItemName">stream</span>, T*<span> </span><span class="keyword keyword apiItemName">devPtr</span>, size_t<span> </span><span class="keyword keyword apiItemName">length</span> = <span class="ph ph apiData">0</span>, unsigned int <span> </span><span class="keyword keyword apiItemName">flags</span> = <span class="ph ph apiData">cudaMemAttachSingle</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">Attach memory to a stream asynchronously. </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">stream</span></tt></dt>
<dd>- Stream in which to enqueue the attach operation </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">devPtr</span></tt></dt>
<dd>- Pointer to memory (must be a pointer to managed memory) </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">length</span></tt></dt>
<dd>- Length of memory (must be zero, defaults to zero) </dd>
<dt><tt class="code"><span class="keyword keyword apiItemName">flags</span></tt></dt>
<dd>- Must be one of <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">cudaMemAttachHost</a> or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">cudaMemAttachSingle</a> (defaults to <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">cudaMemAttachSingle</a>)
</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038285d0c852ab65b8925505e1065563f6d" shape="rect">cudaErrorNotReady</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e00383e8aef5398ee38e28ed41e357b48917c" shape="rect">cudaErrorInvalidValue</a><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038c4673247aee4d1ab8d07871f376e0273" shape="rect">cudaErrorInvalidResourceHandle</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Enqueues an operation in <tt class="ph tt code">stream</tt> to specify stream association of <tt class="ph tt code">length</tt> bytes of memory starting from <tt class="ph tt code">devPtr</tt>. This function is a stream-ordered operation, meaning that it is dependent on, and will only take effect when, previous work
in stream has completed. Any previous association is automatically replaced.
</p>
<p class="p"><tt class="ph tt code">devPtr</tt> must point to an address within managed memory space declared using the __managed__ keyword or allocated with <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" title="Allocates memory that will be automatically managed by the Unified Memory system." shape="rect">cudaMallocManaged</a>.
</p>
<p class="p"><tt class="ph tt code">length</tt> must be zero, to indicate that the entire allocation's stream association is being changed. Currently, it's not possible
to change stream association for a portion of an allocation. The default value for <tt class="ph tt code">length</tt> is zero.
</p>
<p class="p">The stream association is specified using <tt class="ph tt code">flags</tt> which must be one of <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">cudaMemAttachHost</a> or <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">cudaMemAttachSingle</a>. The default value for <tt class="ph tt code">flags</tt> is <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">cudaMemAttachSingle</a> If the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a> flag is specified, the memory can be accessed by any stream on any device. If the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">cudaMemAttachHost</a> flag is specified, the program makes a guarantee that it won't access the memory on the device from any stream. If the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">cudaMemAttachSingle</a> flag is specified, the program makes a guarantee that it will only access the memory on the device from <tt class="ph tt code">stream</tt>. It is illegal to attach singly to the NULL stream, because the NULL stream is a virtual global stream and not a specific
stream. An error will be returned in this case.
</p>
<p class="p">When memory is associated with a single stream, the Unified Memory system will allow CPU access to this memory region so long
as all operations in <tt class="ph tt code">stream</tt> have completed, regardless of whether other streams are active. In effect, this constrains exclusive ownership of the managed
memory region by an active GPU to per-stream activity instead of whole-GPU activity.
</p>
<p class="p">Accessing memory on the device from streams that are not associated with it will produce undefined results. No error checking
is performed by the Unified Memory system to ensure that kernels launched into other streams do not access this region.
</p>
<p class="p">It is a program's responsibility to order calls to <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gebe68658a891edc398791a436a8e1d7c" title="Attach memory to a stream asynchronously." shape="rect">cudaStreamAttachMemAsync</a> via events, synchronization or other means to ensure legal access to memory at all times. Data visibility and coherency will
be changed appropriately for all kernels which follow a stream-association change.
</p>
<p class="p">If <tt class="ph tt code">stream</tt> is destroyed while data is associated with it, the association is removed and the association reverts to the default visibility
of the allocation as specified at <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" title="Allocates memory that will be automatically managed by the Unified Memory system." shape="rect">cudaMallocManaged</a>. For __managed__ variables, the default association is always <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a>. Note that destroying a stream is an asynchronous operation, and as a result, the change to default association won't happen
until all work in the stream has completed.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1gaf38e6f47265c7da1b02724a5ad565e4" title="Create an asynchronous stream." shape="rect">cudaStreamCreate</a>, <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g2f3e3d8e9b3db7fffde77bdf67de7cf1" title="Create an asynchronous stream." shape="rect">cudaStreamCreateWithFlags</a>, <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g80c62c379f0c3ed8afe31fd0a31ad8a2" title="Make a compute stream wait on an event." shape="rect">cudaStreamWaitEvent</a>, <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1geb3b2f88b7c1cff8b67a998a3a41c179" title="Waits for stream tasks to complete." shape="rect">cudaStreamSynchronize</a>, <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g4d2688e1c3f3cf7da4bf55121fc0b0a1" title="Add a callback to a compute stream." shape="rect">cudaStreamAddCallback</a>, <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g796279185cb0335f9cb4aee25b37d01e" title="Destroys and cleans up an asynchronous stream." shape="rect">cudaStreamDestroy</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g37fce6586d509ebd0a4b5f4faa7f3489" title="Allocates memory that will be automatically managed by the Unified Memory system." shape="rect">cudaMallocManaged</a></p>
<p class="p"></p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" id="group__CUDART__HIGHLEVEL_1g1c9273b8f04336f58ec73842f08fb25b" shape="rect">
<!-- --></a><p class="template">template < class T, int dim, enum cudaTextureReadMode readMode ></p><span><a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" title="" shape="rect">cudaError_t</a> cudaUnbindTexture ( const texture < T, dim, readMode > &<span> </span><span class="keyword keyword apiItemName">tex</span> ) [inline] </span></dt>
<dd class="description">
<div class="section">[C++ API] Unbinds a texture </div>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">tex</span></tt></dt>
<dd>- Texture to unbind</dd>
</dl>
</div>
<div class="section">
<h6 class="return_header">Returns</h6>
<p class="return"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a></p>
</div>
<div class="section">
<h6 class="description_header">Description</h6>
<p>Unbinds the texture bound to <tt class="ph tt code">tex</tt>.
</p>
<p class="p"></p>
<p class="p"></p>
<p class="p">
<div class="note note"><span class="notetitle">Note:</span><p class="p">Note that this function may also return error codes from previous, asynchronous launches.</p>
</div>
</p>
<p class="p"></p>
<p class="p apiDesc_subtitle"><strong class="ph b">See also:</strong></p>
<p class="p see_subsection"><a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ga1a74e4296134312d6f117a936bcf2c7" title="[C++ API] Returns a channel descriptor using the specified format" shape="rect">cudaCreateChannelDesc ( C++ API)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g59b47671c6f0ec47408824118d471629" title="Get the channel descriptor of an array." shape="rect">cudaGetChannelDesc</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1g2caa86a0bf6975b64c0028462301924c" title="Get the texture reference associated with a symbol." shape="rect">cudaGetTextureReference</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1ge519938394a575b306290e05ec12102b" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g2aeb95eab6b9d90bb00b26406a27c515" title="[C++ API] Binds a memory area to a texture" shape="rect">cudaBindTexture ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5ae4e8e2d6a28ed3e78caa9a7e853b76" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g67660ae3e9a1ff520575394f78087bea" title="[C++ API] Binds a 2D memory area to a texture" shape="rect">cudaBindTexture2D ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g83bf6619173b5fe0c961a938b6df0816" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g8d9df3146f61cce6231f4512b195d045" title="[C++ API] Binds an array to a texture" shape="rect">cudaBindTextureToArray ( C++ API, inherited channel descriptor)</a>, <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1gfa1b9c9e178a98d64bb648443cc4004a" title="Unbinds a texture." shape="rect">cudaUnbindTexture ( C API)</a>, <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g0beb56df79e50d3e4b1b86adeb2c10bc" title="[C++ API] Get the alignment offset of a texture" shape="rect">cudaGetTextureAlignmentOffset ( C++ API)</a></p>
<p class="p"></p>
</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
>
1165
