diff options
author | David Monahan <david.monahan@arm.com> | 2023-03-22 16:48:58 +0000 |
---|---|---|
committer | David Monahan <david.monahan@arm.com> | 2023-03-22 16:48:58 +0000 |
commit | ae050524109f1ce827962665436ef7430f2ac479 (patch) | |
tree | a087fe0c77570971dd7979f2757426c24e91afc7 /23.02/_open_cl_timer_8cpp_source.xhtml | |
parent | 8d2ca734165a068478df7cffa46185680b05cd20 (diff) | |
download | armnn-ae050524109f1ce827962665436ef7430f2ac479.tar.gz |
IVGCVSW-7255 Update Doxygen Documentation and publish on GitHub.
* Updating Doxygen documentation for 23.02 release.
Signed-off-by: David Monahan <david.monahan@arm.com>
Change-Id: I545574ff7664b4595d2fe6a91a3c35d2ad55df82
Diffstat (limited to '23.02/_open_cl_timer_8cpp_source.xhtml')
-rw-r--r-- | 23.02/_open_cl_timer_8cpp_source.xhtml | 164 |
1 files changed, 144 insertions, 20 deletions
diff --git a/23.02/_open_cl_timer_8cpp_source.xhtml b/23.02/_open_cl_timer_8cpp_source.xhtml index adabcc7691..01ed82327e 100644 --- a/23.02/_open_cl_timer_8cpp_source.xhtml +++ b/23.02/_open_cl_timer_8cpp_source.xhtml @@ -8,7 +8,7 @@ <head> <meta http-equiv="Content-Type" content="text/xhtml;charset=UTF-8"/> <meta http-equiv="X-UA-Compatible" content="IE=9"/> -<meta name="generator" content="Doxygen 1.8.13"/> +<meta name="generator" content="Doxygen 1.8.17"/> <meta name="robots" content="NOINDEX, NOFOLLOW" /> <meta name="viewport" content="width=device-width, initial-scale=1"/> <title>ArmNN: src/backends/cl/OpenClTimer.cpp Source File</title> @@ -19,9 +19,6 @@ <script type="text/javascript" src="resize.js"></script> <script type="text/javascript" src="navtreedata.js"></script> <script type="text/javascript" src="navtree.js"></script> -<script type="text/javascript"> - $(document).ready(initResizable); -</script> <link href="search/search.css" rel="stylesheet" type="text/css"/> <script type="text/javascript" src="search/searchdata.js"></script> <script type="text/javascript" src="search/search.js"></script> @@ -30,7 +27,8 @@ extensions: ["tex2jax.js"], jax: ["input/TeX","output/HTML-CSS"], }); -</script><script type="text/javascript" src="http://cdn.mathjax.org/mathjax/latest/MathJax.js"></script> +</script> +<script type="text/javascript" async="async" src="http://cdn.mathjax.org/mathjax/latest/MathJax.js"></script> <link href="doxygen.css" rel="stylesheet" type="text/css" /> <link href="stylesheet.css" rel="stylesheet" type="text/css"/> </head> @@ -51,18 +49,21 @@ </table> </div> <!-- end header part --> -<!-- Generated by Doxygen 1.8.13 --> +<!-- Generated by Doxygen 1.8.17 --> <script type="text/javascript"> +/* @license magnet:?xt=urn:btih:cf05388f2679ee054f2beb29a391d25f4e673ac3&dn=gpl-2.0.txt GPL-v2 */ var searchBox = new SearchBox("searchBox", "search",false,'Search'); +/* @license-end */ </script> <script type="text/javascript" src="menudata.js"></script> <script type="text/javascript" src="menu.js"></script> <script type="text/javascript"> +/* @license magnet:?xt=urn:btih:cf05388f2679ee054f2beb29a391d25f4e673ac3&dn=gpl-2.0.txt GPL-v2 */ $(function() { initMenu('',true,false,'search.php','Search'); $(document).ready(function() { init_search(); }); }); -</script> +/* @license-end */</script> <div id="main-nav"></div> </div><!-- top --> <div id="side-nav" class="ui-resizable side-nav-resizable"> @@ -76,7 +77,9 @@ $(function() { </div> </div> <script type="text/javascript"> -$(document).ready(function(){initNavTree('_open_cl_timer_8cpp_source.xhtml','');}); +/* @license magnet:?xt=urn:btih:cf05388f2679ee054f2beb29a391d25f4e673ac3&dn=gpl-2.0.txt GPL-v2 */ +$(document).ready(function(){initNavTree('_open_cl_timer_8cpp_source.xhtml',''); initResizable(); }); +/* @license-end */ </script> <div id="doc-content"> <!-- window showing the filter options --> @@ -98,25 +101,146 @@ $(document).ready(function(){initNavTree('_open_cl_timer_8cpp_source.xhtml',''); <div class="title">OpenClTimer.cpp</div> </div> </div><!--header--> <div class="contents"> -<a href="_open_cl_timer_8cpp.xhtml">Go to the documentation of this file.</a><div class="fragment"><div class="line"><a name="l00001"></a><span class="lineno"> 1</span> <span class="comment">//</span></div><div class="line"><a name="l00002"></a><span class="lineno"> 2</span> <span class="comment">// Copyright © 2017 Arm Ltd. All rights reserved.</span></div><div class="line"><a name="l00003"></a><span class="lineno"> 3</span> <span class="comment">// SPDX-License-Identifier: MIT</span></div><div class="line"><a name="l00004"></a><span class="lineno"> 4</span> <span class="comment">//</span></div><div class="line"><a name="l00005"></a><span class="lineno"> 5</span> </div><div class="line"><a name="l00006"></a><span class="lineno"> 6</span> <span class="preprocessor">#include "<a class="code" href="_open_cl_timer_8hpp.xhtml">OpenClTimer.hpp</a>"</span></div><div class="line"><a name="l00007"></a><span class="lineno"> 7</span> </div><div class="line"><a name="l00008"></a><span class="lineno"> 8</span> <span class="preprocessor">#include <<a class="code" href="_ignore_unused_8hpp.xhtml">armnn/utility/IgnoreUnused.hpp</a>></span></div><div class="line"><a name="l00009"></a><span class="lineno"> 9</span> </div><div class="line"><a name="l00010"></a><span class="lineno"> 10</span> <span class="preprocessor">#include <string></span></div><div class="line"><a name="l00011"></a><span class="lineno"> 11</span> <span class="preprocessor">#include <sstream></span></div><div class="line"><a name="l00012"></a><span class="lineno"> 12</span> </div><div class="line"><a name="l00013"></a><span class="lineno"> 13</span> </div><div class="line"><a name="l00014"></a><span class="lineno"> 14</span> <span class="keyword">namespace </span><a class="code" href="namespacearmnn.xhtml">armnn</a></div><div class="line"><a name="l00015"></a><span class="lineno"> 15</span> {</div><div class="line"><a name="l00016"></a><span class="lineno"> 16</span> </div><div class="line"><a name="l00017"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#adcd19a0c31e8ffa4411fa05e905c0cf4"> 17</a></span> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#adcd19a0c31e8ffa4411fa05e905c0cf4">OpenClTimer::OpenClTimer</a>()</div><div class="line"><a name="l00018"></a><span class="lineno"> 18</span> {</div><div class="line"><a name="l00019"></a><span class="lineno"> 19</span> }</div><div class="line"><a name="l00020"></a><span class="lineno"> 20</span> </div><div class="line"><a name="l00021"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#a156f3866ca69d98b4d9e6e1c1b3ec7da"> 21</a></span> <span class="keywordtype">void</span> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#a156f3866ca69d98b4d9e6e1c1b3ec7da">OpenClTimer::Start</a>()</div><div class="line"><a name="l00022"></a><span class="lineno"> 22</span> {</div><div class="line"><a name="l00023"></a><span class="lineno"> 23</span>  m_Kernels.clear();</div><div class="line"><a name="l00024"></a><span class="lineno"> 24</span> </div><div class="line"><a name="l00025"></a><span class="lineno"> 25</span>  <span class="keyword">auto</span> interceptor = [<span class="keyword">this</span>]( cl_command_queue command_queue,</div><div class="line"><a name="l00026"></a><span class="lineno"> 26</span>  cl_kernel kernel,</div><div class="line"><a name="l00027"></a><span class="lineno"> 27</span>  cl_uint work_dim,</div><div class="line"><a name="l00028"></a><span class="lineno"> 28</span>  <span class="keyword">const</span> <span class="keywordtype">size_t</span> *gwo,</div><div class="line"><a name="l00029"></a><span class="lineno"> 29</span>  <span class="keyword">const</span> <span class="keywordtype">size_t</span> *gws,</div><div class="line"><a name="l00030"></a><span class="lineno"> 30</span>  <span class="keyword">const</span> <span class="keywordtype">size_t</span> *lws,</div><div class="line"><a name="l00031"></a><span class="lineno"> 31</span>  cl_uint num_events_in_wait_list,</div><div class="line"><a name="l00032"></a><span class="lineno"> 32</span>  <span class="keyword">const</span> cl_event * event_wait_list,</div><div class="line"><a name="l00033"></a><span class="lineno"> 33</span>  cl_event * event)</div><div class="line"><a name="l00034"></a><span class="lineno"> 34</span>  {</div><div class="line"><a name="l00035"></a><span class="lineno"> 35</span>  <a class="code" href="namespacearmnn.xhtml#a44affeeb090c3c6a3062830562672e84">IgnoreUnused</a>(event);</div><div class="line"><a name="l00036"></a><span class="lineno"> 36</span>  cl_int retVal = 0;</div><div class="line"><a name="l00037"></a><span class="lineno"> 37</span> </div><div class="line"><a name="l00038"></a><span class="lineno"> 38</span>  <span class="comment">// Get the name of the kernel</span></div><div class="line"><a name="l00039"></a><span class="lineno"> 39</span>  cl::Kernel retainedKernel(kernel, <span class="keyword">true</span>);</div><div class="line"><a name="l00040"></a><span class="lineno"> 40</span>  std::stringstream ss;</div><div class="line"><a name="l00041"></a><span class="lineno"> 41</span>  ss << retainedKernel.getInfo<CL_KERNEL_FUNCTION_NAME>();</div><div class="line"><a name="l00042"></a><span class="lineno"> 42</span> </div><div class="line"><a name="l00043"></a><span class="lineno"> 43</span>  <span class="comment">// Embed workgroup sizes into the name</span></div><div class="line"><a name="l00044"></a><span class="lineno"> 44</span>  <span class="keywordflow">if</span>(gws != <span class="keyword">nullptr</span>)</div><div class="line"><a name="l00045"></a><span class="lineno"> 45</span>  {</div><div class="line"><a name="l00046"></a><span class="lineno"> 46</span>  ss << <span class="stringliteral">" GWS["</span> << gws[0] << <span class="stringliteral">","</span> << gws[1] << <span class="stringliteral">","</span> << gws[2] << <span class="stringliteral">"]"</span>;</div><div class="line"><a name="l00047"></a><span class="lineno"> 47</span>  }</div><div class="line"><a name="l00048"></a><span class="lineno"> 48</span>  <span class="keywordflow">if</span>(lws != <span class="keyword">nullptr</span>)</div><div class="line"><a name="l00049"></a><span class="lineno"> 49</span>  {</div><div class="line"><a name="l00050"></a><span class="lineno"> 50</span>  ss << <span class="stringliteral">" LWS["</span> << lws[0] << <span class="stringliteral">","</span> << lws[1] << <span class="stringliteral">","</span> << lws[2] << <span class="stringliteral">"]"</span>;</div><div class="line"><a name="l00051"></a><span class="lineno"> 51</span>  }</div><div class="line"><a name="l00052"></a><span class="lineno"> 52</span> </div><div class="line"><a name="l00053"></a><span class="lineno"> 53</span>  cl_event customEvent;</div><div class="line"><a name="l00054"></a><span class="lineno"> 54</span> </div><div class="line"><a name="l00055"></a><span class="lineno"> 55</span>  <span class="comment">// Forward to original OpenCl function</span></div><div class="line"><a name="l00056"></a><span class="lineno"> 56</span>  retVal = m_OriginalEnqueueFunction( command_queue,</div><div class="line"><a name="l00057"></a><span class="lineno"> 57</span>  kernel,</div><div class="line"><a name="l00058"></a><span class="lineno"> 58</span>  work_dim,</div><div class="line"><a name="l00059"></a><span class="lineno"> 59</span>  gwo,</div><div class="line"><a name="l00060"></a><span class="lineno"> 60</span>  gws,</div><div class="line"><a name="l00061"></a><span class="lineno"> 61</span>  lws,</div><div class="line"><a name="l00062"></a><span class="lineno"> 62</span>  num_events_in_wait_list,</div><div class="line"><a name="l00063"></a><span class="lineno"> 63</span>  event_wait_list,</div><div class="line"><a name="l00064"></a><span class="lineno"> 64</span>  &customEvent);</div><div class="line"><a name="l00065"></a><span class="lineno"> 65</span> </div><div class="line"><a name="l00066"></a><span class="lineno"> 66</span>  <span class="comment">// Store the Kernel info for later GetMeasurements() call</span></div><div class="line"><a name="l00067"></a><span class="lineno"> 67</span>  m_Kernels.emplace_back(ss.str(), customEvent);</div><div class="line"><a name="l00068"></a><span class="lineno"> 68</span> </div><div class="line"><a name="l00069"></a><span class="lineno"> 69</span>  <span class="keywordflow">if</span>(event != <span class="keyword">nullptr</span>)</div><div class="line"><a name="l00070"></a><span class="lineno"> 70</span>  {</div><div class="line"><a name="l00071"></a><span class="lineno"> 71</span>  <span class="comment">//return cl_event from the intercepted call</span></div><div class="line"><a name="l00072"></a><span class="lineno"> 72</span>  clRetainEvent(customEvent);</div><div class="line"><a name="l00073"></a><span class="lineno"> 73</span>  *<span class="keyword">event</span> = customEvent;</div><div class="line"><a name="l00074"></a><span class="lineno"> 74</span>  }</div><div class="line"><a name="l00075"></a><span class="lineno"> 75</span> </div><div class="line"><a name="l00076"></a><span class="lineno"> 76</span>  <span class="keywordflow">return</span> retVal;</div><div class="line"><a name="l00077"></a><span class="lineno"> 77</span>  };</div><div class="line"><a name="l00078"></a><span class="lineno"> 78</span> </div><div class="line"><a name="l00079"></a><span class="lineno"> 79</span>  m_OriginalEnqueueFunction = CLSymbols::get().clEnqueueNDRangeKernel_ptr;</div><div class="line"><a name="l00080"></a><span class="lineno"> 80</span>  CLSymbols::get().clEnqueueNDRangeKernel_ptr = interceptor;</div><div class="line"><a name="l00081"></a><span class="lineno"> 81</span> }</div><div class="line"><a name="l00082"></a><span class="lineno"> 82</span> </div><div class="line"><a name="l00083"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#a634c58de2126b4a4e6a2a093e60e1290"> 83</a></span> <span class="keywordtype">void</span> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#a634c58de2126b4a4e6a2a093e60e1290">OpenClTimer::Stop</a>()</div><div class="line"><a name="l00084"></a><span class="lineno"> 84</span> {</div><div class="line"><a name="l00085"></a><span class="lineno"> 85</span>  CLSymbols::get().clEnqueueNDRangeKernel_ptr = m_OriginalEnqueueFunction;</div><div class="line"><a name="l00086"></a><span class="lineno"> 86</span> }</div><div class="line"><a name="l00087"></a><span class="lineno"> 87</span> </div><div class="line"><a name="l00088"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#ae9faa4ff4d8569776b5686e472c46bb0"> 88</a></span> <span class="keywordtype">bool</span> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#ae9faa4ff4d8569776b5686e472c46bb0">OpenClTimer::HasKernelMeasurements</a>()<span class="keyword"> const</span></div><div class="line"><a name="l00089"></a><span class="lineno"> 89</span> <span class="keyword"></span>{</div><div class="line"><a name="l00090"></a><span class="lineno"> 90</span>  <span class="keywordflow">return</span> m_Kernels.size() > 0;</div><div class="line"><a name="l00091"></a><span class="lineno"> 91</span> }</div><div class="line"><a name="l00092"></a><span class="lineno"> 92</span> </div><div class="line"><a name="l00093"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#a86ea36032637c02c045f2d433036a203"> 93</a></span> std::vector<Measurement> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#a86ea36032637c02c045f2d433036a203">OpenClTimer::GetMeasurements</a>()<span class="keyword"> const</span></div><div class="line"><a name="l00094"></a><span class="lineno"> 94</span> <span class="keyword"></span>{</div><div class="line"><a name="l00095"></a><span class="lineno"> 95</span>  std::vector<Measurement> measurements;</div><div class="line"><a name="l00096"></a><span class="lineno"> 96</span> </div><div class="line"><a name="l00097"></a><span class="lineno"> 97</span>  cl_command_queue_properties clQueueProperties = CLScheduler::get().queue().getInfo<CL_QUEUE_PROPERTIES>();</div><div class="line"><a name="l00098"></a><span class="lineno"> 98</span> </div><div class="line"><a name="l00099"></a><span class="lineno"> 99</span>  <span class="keywordtype">int</span> idx = 0;</div><div class="line"><a name="l00100"></a><span class="lineno"> 100</span>  <span class="keywordflow">for</span> (<span class="keyword">auto</span>& kernel : m_Kernels)</div><div class="line"><a name="l00101"></a><span class="lineno"> 101</span>  {</div><div class="line"><a name="l00102"></a><span class="lineno"> 102</span>  std::string name = std::string(this-><a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#a7ddf0cf6f620d59c10e63495ace795d0">GetName</a>()) + <span class="stringliteral">"/"</span> + std::to_string(idx++) + <span class="stringliteral">": "</span> + kernel.m_Name;</div><div class="line"><a name="l00103"></a><span class="lineno"> 103</span> </div><div class="line"><a name="l00104"></a><span class="lineno"> 104</span>  <span class="keywordtype">double</span> timeUs = 0.0;</div><div class="line"><a name="l00105"></a><span class="lineno"> 105</span>  <span class="keywordflow">if</span>((clQueueProperties & CL_QUEUE_PROFILING_ENABLE) != 0)</div><div class="line"><a name="l00106"></a><span class="lineno"> 106</span>  {</div><div class="line"><a name="l00107"></a><span class="lineno"> 107</span>  <span class="comment">// Wait for the event to finish before accessing profile results.</span></div><div class="line"><a name="l00108"></a><span class="lineno"> 108</span>  kernel.m_Event.wait();</div><div class="line"><a name="l00109"></a><span class="lineno"> 109</span> </div><div class="line"><a name="l00110"></a><span class="lineno"> 110</span>  cl_ulong start = kernel.m_Event.getProfilingInfo<CL_PROFILING_COMMAND_START>();</div><div class="line"><a name="l00111"></a><span class="lineno"> 111</span>  cl_ulong end = kernel.m_Event.getProfilingInfo<CL_PROFILING_COMMAND_END>();</div><div class="line"><a name="l00112"></a><span class="lineno"> 112</span>  timeUs = <span class="keyword">static_cast<</span><span class="keywordtype">double</span><span class="keyword">></span>(end - start) / 1000.0;</div><div class="line"><a name="l00113"></a><span class="lineno"> 113</span>  }</div><div class="line"><a name="l00114"></a><span class="lineno"> 114</span> </div><div class="line"><a name="l00115"></a><span class="lineno"> 115</span>  measurements.emplace_back(name, timeUs, Measurement::Unit::TIME_US);</div><div class="line"><a name="l00116"></a><span class="lineno"> 116</span>  }</div><div class="line"><a name="l00117"></a><span class="lineno"> 117</span> </div><div class="line"><a name="l00118"></a><span class="lineno"> 118</span>  <span class="keywordflow">return</span> measurements;</div><div class="line"><a name="l00119"></a><span class="lineno"> 119</span> }</div><div class="line"><a name="l00120"></a><span class="lineno"> 120</span> </div><div class="line"><a name="l00121"></a><span class="lineno"> 121</span> } <span class="comment">//namespace armnn</span></div><div class="ttc" id="classarmnn_1_1_open_cl_timer_xhtml_ae9faa4ff4d8569776b5686e472c46bb0"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#ae9faa4ff4d8569776b5686e472c46bb0">armnn::OpenClTimer::HasKernelMeasurements</a></div><div class="ttdeci">bool HasKernelMeasurements() const override</div><div class="ttdoc">Return true if this Instrument has kernels for recording measurements. </div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00088">OpenClTimer.cpp:88</a></div></div> -<div class="ttc" id="_ignore_unused_8hpp_xhtml"><div class="ttname"><a href="_ignore_unused_8hpp.xhtml">IgnoreUnused.hpp</a></div></div> -<div class="ttc" id="classarmnn_1_1_open_cl_timer_xhtml_a156f3866ca69d98b4d9e6e1c1b3ec7da"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#a156f3866ca69d98b4d9e6e1c1b3ec7da">armnn::OpenClTimer::Start</a></div><div class="ttdeci">void Start() override</div><div class="ttdoc">Start the OpenCl timer. </div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00021">OpenClTimer.cpp:21</a></div></div> -<div class="ttc" id="classarmnn_1_1_open_cl_timer_xhtml_a634c58de2126b4a4e6a2a093e60e1290"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#a634c58de2126b4a4e6a2a093e60e1290">armnn::OpenClTimer::Stop</a></div><div class="ttdeci">void Stop() override</div><div class="ttdoc">Stop the OpenCl timer. </div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00083">OpenClTimer.cpp:83</a></div></div> -<div class="ttc" id="namespacearmnn_xhtml"><div class="ttname"><a href="namespacearmnn.xhtml">armnn</a></div><div class="ttdoc">Copyright (c) 2021 ARM Limited and Contributors. </div><div class="ttdef"><b>Definition:</b> <a href="01__00__quick__start_8dox_source.xhtml#l00006">01_00_quick_start.dox:6</a></div></div> -<div class="ttc" id="namespacearmnn_xhtml_a44affeeb090c3c6a3062830562672e84"><div class="ttname"><a href="namespacearmnn.xhtml#a44affeeb090c3c6a3062830562672e84">armnn::IgnoreUnused</a></div><div class="ttdeci">void IgnoreUnused(Ts &&...)</div><div class="ttdef"><b>Definition:</b> <a href="_ignore_unused_8hpp_source.xhtml#l00014">IgnoreUnused.hpp:14</a></div></div> -<div class="ttc" id="_open_cl_timer_8hpp_xhtml"><div class="ttname"><a href="_open_cl_timer_8hpp.xhtml">OpenClTimer.hpp</a></div></div> -<div class="ttc" id="classarmnn_1_1_open_cl_timer_xhtml_a86ea36032637c02c045f2d433036a203"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#a86ea36032637c02c045f2d433036a203">armnn::OpenClTimer::GetMeasurements</a></div><div class="ttdeci">std::vector< Measurement > GetMeasurements() const override</div><div class="ttdoc">Get the recorded measurements. </div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00093">OpenClTimer.cpp:93</a></div></div> -<div class="ttc" id="classarmnn_1_1_open_cl_timer_xhtml_a7ddf0cf6f620d59c10e63495ace795d0"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#a7ddf0cf6f620d59c10e63495ace795d0">armnn::OpenClTimer::GetName</a></div><div class="ttdeci">const char * GetName() const override</div><div class="ttdoc">Get the name of the timer. </div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8hpp_source.xhtml#l00037">OpenClTimer.hpp:37</a></div></div> -<div class="ttc" id="classarmnn_1_1_open_cl_timer_xhtml_adcd19a0c31e8ffa4411fa05e905c0cf4"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#adcd19a0c31e8ffa4411fa05e905c0cf4">armnn::OpenClTimer::OpenClTimer</a></div><div class="ttdeci">OpenClTimer()</div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00017">OpenClTimer.cpp:17</a></div></div> +<a href="_open_cl_timer_8cpp.xhtml">Go to the documentation of this file.</a><div class="fragment"><div class="line"><a name="l00001"></a><span class="lineno"> 1</span> <span class="comment">//</span></div> +<div class="line"><a name="l00002"></a><span class="lineno"> 2</span> <span class="comment">// Copyright © 2017 Arm Ltd. All rights reserved.</span></div> +<div class="line"><a name="l00003"></a><span class="lineno"> 3</span> <span class="comment">// SPDX-License-Identifier: MIT</span></div> +<div class="line"><a name="l00004"></a><span class="lineno"> 4</span> <span class="comment">//</span></div> +<div class="line"><a name="l00005"></a><span class="lineno"> 5</span>  </div> +<div class="line"><a name="l00006"></a><span class="lineno"> 6</span> <span class="preprocessor">#include "<a class="code" href="_open_cl_timer_8hpp.xhtml">OpenClTimer.hpp</a>"</span></div> +<div class="line"><a name="l00007"></a><span class="lineno"> 7</span>  </div> +<div class="line"><a name="l00008"></a><span class="lineno"> 8</span> <span class="preprocessor">#include <<a class="code" href="_ignore_unused_8hpp.xhtml">armnn/utility/IgnoreUnused.hpp</a>></span></div> +<div class="line"><a name="l00009"></a><span class="lineno"> 9</span>  </div> +<div class="line"><a name="l00010"></a><span class="lineno"> 10</span> <span class="preprocessor">#include <string></span></div> +<div class="line"><a name="l00011"></a><span class="lineno"> 11</span> <span class="preprocessor">#include <sstream></span></div> +<div class="line"><a name="l00012"></a><span class="lineno"> 12</span>  </div> +<div class="line"><a name="l00013"></a><span class="lineno"> 13</span>  </div> +<div class="line"><a name="l00014"></a><span class="lineno"> 14</span> <span class="keyword">namespace </span><a class="code" href="namespacearmnn.xhtml">armnn</a></div> +<div class="line"><a name="l00015"></a><span class="lineno"> 15</span> {</div> +<div class="line"><a name="l00016"></a><span class="lineno"> 16</span>  </div> +<div class="line"><a name="l00017"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#adcd19a0c31e8ffa4411fa05e905c0cf4"> 17</a></span> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#adcd19a0c31e8ffa4411fa05e905c0cf4">OpenClTimer::OpenClTimer</a>()</div> +<div class="line"><a name="l00018"></a><span class="lineno"> 18</span> {</div> +<div class="line"><a name="l00019"></a><span class="lineno"> 19</span> }</div> +<div class="line"><a name="l00020"></a><span class="lineno"> 20</span>  </div> +<div class="line"><a name="l00021"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#a156f3866ca69d98b4d9e6e1c1b3ec7da"> 21</a></span> <span class="keywordtype">void</span> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#a156f3866ca69d98b4d9e6e1c1b3ec7da">OpenClTimer::Start</a>()</div> +<div class="line"><a name="l00022"></a><span class="lineno"> 22</span> {</div> +<div class="line"><a name="l00023"></a><span class="lineno"> 23</span>  m_Kernels.clear();</div> +<div class="line"><a name="l00024"></a><span class="lineno"> 24</span>  </div> +<div class="line"><a name="l00025"></a><span class="lineno"> 25</span>  <span class="keyword">auto</span> interceptor = [<span class="keyword">this</span>]( cl_command_queue command_queue,</div> +<div class="line"><a name="l00026"></a><span class="lineno"> 26</span>  cl_kernel kernel,</div> +<div class="line"><a name="l00027"></a><span class="lineno"> 27</span>  cl_uint work_dim,</div> +<div class="line"><a name="l00028"></a><span class="lineno"> 28</span>  <span class="keyword">const</span> <span class="keywordtype">size_t</span> *gwo,</div> +<div class="line"><a name="l00029"></a><span class="lineno"> 29</span>  <span class="keyword">const</span> <span class="keywordtype">size_t</span> *gws,</div> +<div class="line"><a name="l00030"></a><span class="lineno"> 30</span>  <span class="keyword">const</span> <span class="keywordtype">size_t</span> *lws,</div> +<div class="line"><a name="l00031"></a><span class="lineno"> 31</span>  cl_uint num_events_in_wait_list,</div> +<div class="line"><a name="l00032"></a><span class="lineno"> 32</span>  <span class="keyword">const</span> cl_event * event_wait_list,</div> +<div class="line"><a name="l00033"></a><span class="lineno"> 33</span>  cl_event * event)</div> +<div class="line"><a name="l00034"></a><span class="lineno"> 34</span>  {</div> +<div class="line"><a name="l00035"></a><span class="lineno"> 35</span>  <a class="code" href="namespacearmnn.xhtml#a44affeeb090c3c6a3062830562672e84">IgnoreUnused</a>(event);</div> +<div class="line"><a name="l00036"></a><span class="lineno"> 36</span>  cl_int retVal = 0;</div> +<div class="line"><a name="l00037"></a><span class="lineno"> 37</span>  </div> +<div class="line"><a name="l00038"></a><span class="lineno"> 38</span>  <span class="comment">// Get the name of the kernel</span></div> +<div class="line"><a name="l00039"></a><span class="lineno"> 39</span>  cl::Kernel retainedKernel(kernel, <span class="keyword">true</span>);</div> +<div class="line"><a name="l00040"></a><span class="lineno"> 40</span>  std::stringstream ss;</div> +<div class="line"><a name="l00041"></a><span class="lineno"> 41</span>  ss << retainedKernel.getInfo<CL_KERNEL_FUNCTION_NAME>();</div> +<div class="line"><a name="l00042"></a><span class="lineno"> 42</span>  </div> +<div class="line"><a name="l00043"></a><span class="lineno"> 43</span>  <span class="comment">// Embed workgroup sizes into the name</span></div> +<div class="line"><a name="l00044"></a><span class="lineno"> 44</span>  <span class="keywordflow">if</span>(gws != <span class="keyword">nullptr</span>)</div> +<div class="line"><a name="l00045"></a><span class="lineno"> 45</span>  {</div> +<div class="line"><a name="l00046"></a><span class="lineno"> 46</span>  ss << <span class="stringliteral">" GWS["</span> << gws[0] << <span class="stringliteral">","</span> << gws[1] << <span class="stringliteral">","</span> << gws[2] << <span class="stringliteral">"]"</span>;</div> +<div class="line"><a name="l00047"></a><span class="lineno"> 47</span>  }</div> +<div class="line"><a name="l00048"></a><span class="lineno"> 48</span>  <span class="keywordflow">if</span>(lws != <span class="keyword">nullptr</span>)</div> +<div class="line"><a name="l00049"></a><span class="lineno"> 49</span>  {</div> +<div class="line"><a name="l00050"></a><span class="lineno"> 50</span>  ss << <span class="stringliteral">" LWS["</span> << lws[0] << <span class="stringliteral">","</span> << lws[1] << <span class="stringliteral">","</span> << lws[2] << <span class="stringliteral">"]"</span>;</div> +<div class="line"><a name="l00051"></a><span class="lineno"> 51</span>  }</div> +<div class="line"><a name="l00052"></a><span class="lineno"> 52</span>  </div> +<div class="line"><a name="l00053"></a><span class="lineno"> 53</span>  cl_event customEvent;</div> +<div class="line"><a name="l00054"></a><span class="lineno"> 54</span>  </div> +<div class="line"><a name="l00055"></a><span class="lineno"> 55</span>  <span class="comment">// Forward to original OpenCl function</span></div> +<div class="line"><a name="l00056"></a><span class="lineno"> 56</span>  retVal = m_OriginalEnqueueFunction( command_queue,</div> +<div class="line"><a name="l00057"></a><span class="lineno"> 57</span>  kernel,</div> +<div class="line"><a name="l00058"></a><span class="lineno"> 58</span>  work_dim,</div> +<div class="line"><a name="l00059"></a><span class="lineno"> 59</span>  gwo,</div> +<div class="line"><a name="l00060"></a><span class="lineno"> 60</span>  gws,</div> +<div class="line"><a name="l00061"></a><span class="lineno"> 61</span>  lws,</div> +<div class="line"><a name="l00062"></a><span class="lineno"> 62</span>  num_events_in_wait_list,</div> +<div class="line"><a name="l00063"></a><span class="lineno"> 63</span>  event_wait_list,</div> +<div class="line"><a name="l00064"></a><span class="lineno"> 64</span>  &customEvent);</div> +<div class="line"><a name="l00065"></a><span class="lineno"> 65</span>  </div> +<div class="line"><a name="l00066"></a><span class="lineno"> 66</span>  <span class="comment">// Store the Kernel info for later GetMeasurements() call</span></div> +<div class="line"><a name="l00067"></a><span class="lineno"> 67</span>  m_Kernels.emplace_back(ss.str(), customEvent);</div> +<div class="line"><a name="l00068"></a><span class="lineno"> 68</span>  </div> +<div class="line"><a name="l00069"></a><span class="lineno"> 69</span>  <span class="keywordflow">if</span>(event != <span class="keyword">nullptr</span>)</div> +<div class="line"><a name="l00070"></a><span class="lineno"> 70</span>  {</div> +<div class="line"><a name="l00071"></a><span class="lineno"> 71</span>  <span class="comment">//return cl_event from the intercepted call</span></div> +<div class="line"><a name="l00072"></a><span class="lineno"> 72</span>  clRetainEvent(customEvent);</div> +<div class="line"><a name="l00073"></a><span class="lineno"> 73</span>  *<span class="keyword">event</span> = customEvent;</div> +<div class="line"><a name="l00074"></a><span class="lineno"> 74</span>  }</div> +<div class="line"><a name="l00075"></a><span class="lineno"> 75</span>  </div> +<div class="line"><a name="l00076"></a><span class="lineno"> 76</span>  <span class="keywordflow">return</span> retVal;</div> +<div class="line"><a name="l00077"></a><span class="lineno"> 77</span>  };</div> +<div class="line"><a name="l00078"></a><span class="lineno"> 78</span>  </div> +<div class="line"><a name="l00079"></a><span class="lineno"> 79</span>  m_OriginalEnqueueFunction = CLSymbols::get().clEnqueueNDRangeKernel_ptr;</div> +<div class="line"><a name="l00080"></a><span class="lineno"> 80</span>  CLSymbols::get().clEnqueueNDRangeKernel_ptr = interceptor;</div> +<div class="line"><a name="l00081"></a><span class="lineno"> 81</span> }</div> +<div class="line"><a name="l00082"></a><span class="lineno"> 82</span>  </div> +<div class="line"><a name="l00083"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#a634c58de2126b4a4e6a2a093e60e1290"> 83</a></span> <span class="keywordtype">void</span> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#a634c58de2126b4a4e6a2a093e60e1290">OpenClTimer::Stop</a>()</div> +<div class="line"><a name="l00084"></a><span class="lineno"> 84</span> {</div> +<div class="line"><a name="l00085"></a><span class="lineno"> 85</span>  CLSymbols::get().clEnqueueNDRangeKernel_ptr = m_OriginalEnqueueFunction;</div> +<div class="line"><a name="l00086"></a><span class="lineno"> 86</span> }</div> +<div class="line"><a name="l00087"></a><span class="lineno"> 87</span>  </div> +<div class="line"><a name="l00088"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#ae9faa4ff4d8569776b5686e472c46bb0"> 88</a></span> <span class="keywordtype">bool</span> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#ae9faa4ff4d8569776b5686e472c46bb0">OpenClTimer::HasKernelMeasurements</a>()<span class="keyword"> const</span></div> +<div class="line"><a name="l00089"></a><span class="lineno"> 89</span> <span class="keyword"></span>{</div> +<div class="line"><a name="l00090"></a><span class="lineno"> 90</span>  <span class="keywordflow">return</span> m_Kernels.size() > 0;</div> +<div class="line"><a name="l00091"></a><span class="lineno"> 91</span> }</div> +<div class="line"><a name="l00092"></a><span class="lineno"> 92</span>  </div> +<div class="line"><a name="l00093"></a><span class="lineno"><a class="line" href="classarmnn_1_1_open_cl_timer.xhtml#a86ea36032637c02c045f2d433036a203"> 93</a></span> std::vector<Measurement> <a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#a86ea36032637c02c045f2d433036a203">OpenClTimer::GetMeasurements</a>()<span class="keyword"> const</span></div> +<div class="line"><a name="l00094"></a><span class="lineno"> 94</span> <span class="keyword"></span>{</div> +<div class="line"><a name="l00095"></a><span class="lineno"> 95</span>  std::vector<Measurement> measurements;</div> +<div class="line"><a name="l00096"></a><span class="lineno"> 96</span>  </div> +<div class="line"><a name="l00097"></a><span class="lineno"> 97</span>  cl_command_queue_properties clQueueProperties = CLScheduler::get().queue().getInfo<CL_QUEUE_PROPERTIES>();</div> +<div class="line"><a name="l00098"></a><span class="lineno"> 98</span>  </div> +<div class="line"><a name="l00099"></a><span class="lineno"> 99</span>  <span class="keywordtype">int</span> idx = 0;</div> +<div class="line"><a name="l00100"></a><span class="lineno"> 100</span>  <span class="keywordflow">for</span> (<span class="keyword">auto</span>& kernel : m_Kernels)</div> +<div class="line"><a name="l00101"></a><span class="lineno"> 101</span>  {</div> +<div class="line"><a name="l00102"></a><span class="lineno"> 102</span>  std::string name = std::string(this-><a class="code" href="classarmnn_1_1_open_cl_timer.xhtml#a7ddf0cf6f620d59c10e63495ace795d0">GetName</a>()) + <span class="stringliteral">"/"</span> + std::to_string(idx++) + <span class="stringliteral">": "</span> + kernel.m_Name;</div> +<div class="line"><a name="l00103"></a><span class="lineno"> 103</span>  </div> +<div class="line"><a name="l00104"></a><span class="lineno"> 104</span>  <span class="keywordtype">double</span> timeUs = 0.0;</div> +<div class="line"><a name="l00105"></a><span class="lineno"> 105</span>  <span class="keywordflow">if</span>((clQueueProperties & CL_QUEUE_PROFILING_ENABLE) != 0)</div> +<div class="line"><a name="l00106"></a><span class="lineno"> 106</span>  {</div> +<div class="line"><a name="l00107"></a><span class="lineno"> 107</span>  <span class="comment">// Wait for the event to finish before accessing profile results.</span></div> +<div class="line"><a name="l00108"></a><span class="lineno"> 108</span>  kernel.m_Event.wait();</div> +<div class="line"><a name="l00109"></a><span class="lineno"> 109</span>  </div> +<div class="line"><a name="l00110"></a><span class="lineno"> 110</span>  cl_ulong start = kernel.m_Event.getProfilingInfo<CL_PROFILING_COMMAND_START>();</div> +<div class="line"><a name="l00111"></a><span class="lineno"> 111</span>  cl_ulong end = kernel.m_Event.getProfilingInfo<CL_PROFILING_COMMAND_END>();</div> +<div class="line"><a name="l00112"></a><span class="lineno"> 112</span>  timeUs = <span class="keyword">static_cast<</span><span class="keywordtype">double</span><span class="keyword">></span>(end - start) / 1000.0;</div> +<div class="line"><a name="l00113"></a><span class="lineno"> 113</span>  }</div> +<div class="line"><a name="l00114"></a><span class="lineno"> 114</span>  </div> +<div class="line"><a name="l00115"></a><span class="lineno"> 115</span>  measurements.emplace_back(name, timeUs, Measurement::Unit::TIME_US);</div> +<div class="line"><a name="l00116"></a><span class="lineno"> 116</span>  }</div> +<div class="line"><a name="l00117"></a><span class="lineno"> 117</span>  </div> +<div class="line"><a name="l00118"></a><span class="lineno"> 118</span>  <span class="keywordflow">return</span> measurements;</div> +<div class="line"><a name="l00119"></a><span class="lineno"> 119</span> }</div> +<div class="line"><a name="l00120"></a><span class="lineno"> 120</span>  </div> +<div class="line"><a name="l00121"></a><span class="lineno"> 121</span> } <span class="comment">//namespace armnn</span></div> </div><!-- fragment --></div><!-- contents --> </div><!-- doc-content --> +<div class="ttc" id="aclassarmnn_1_1_open_cl_timer_xhtml_a7ddf0cf6f620d59c10e63495ace795d0"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#a7ddf0cf6f620d59c10e63495ace795d0">armnn::OpenClTimer::GetName</a></div><div class="ttdeci">const char * GetName() const override</div><div class="ttdoc">Get the name of the timer.</div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8hpp_source.xhtml#l00037">OpenClTimer.hpp:37</a></div></div> +<div class="ttc" id="aclassarmnn_1_1_open_cl_timer_xhtml_a156f3866ca69d98b4d9e6e1c1b3ec7da"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#a156f3866ca69d98b4d9e6e1c1b3ec7da">armnn::OpenClTimer::Start</a></div><div class="ttdeci">void Start() override</div><div class="ttdoc">Start the OpenCl timer.</div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00021">OpenClTimer.cpp:21</a></div></div> +<div class="ttc" id="anamespacearmnn_xhtml_a44affeeb090c3c6a3062830562672e84"><div class="ttname"><a href="namespacearmnn.xhtml#a44affeeb090c3c6a3062830562672e84">armnn::IgnoreUnused</a></div><div class="ttdeci">void IgnoreUnused(Ts &&...)</div><div class="ttdef"><b>Definition:</b> <a href="_ignore_unused_8hpp_source.xhtml#l00014">IgnoreUnused.hpp:14</a></div></div> +<div class="ttc" id="anamespacearmnn_xhtml"><div class="ttname"><a href="namespacearmnn.xhtml">armnn</a></div><div class="ttdoc">Copyright (c) 2021 ARM Limited and Contributors.</div><div class="ttdef"><b>Definition:</b> <a href="01__00__quick__start_8dox_source.xhtml#l00006">01_00_quick_start.dox:6</a></div></div> +<div class="ttc" id="aclassarmnn_1_1_open_cl_timer_xhtml_a634c58de2126b4a4e6a2a093e60e1290"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#a634c58de2126b4a4e6a2a093e60e1290">armnn::OpenClTimer::Stop</a></div><div class="ttdeci">void Stop() override</div><div class="ttdoc">Stop the OpenCl timer.</div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00083">OpenClTimer.cpp:83</a></div></div> +<div class="ttc" id="a_open_cl_timer_8hpp_xhtml"><div class="ttname"><a href="_open_cl_timer_8hpp.xhtml">OpenClTimer.hpp</a></div></div> +<div class="ttc" id="aclassarmnn_1_1_open_cl_timer_xhtml_ae9faa4ff4d8569776b5686e472c46bb0"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#ae9faa4ff4d8569776b5686e472c46bb0">armnn::OpenClTimer::HasKernelMeasurements</a></div><div class="ttdeci">bool HasKernelMeasurements() const override</div><div class="ttdoc">Return true if this Instrument has kernels for recording measurements.</div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00088">OpenClTimer.cpp:88</a></div></div> +<div class="ttc" id="aclassarmnn_1_1_open_cl_timer_xhtml_a86ea36032637c02c045f2d433036a203"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#a86ea36032637c02c045f2d433036a203">armnn::OpenClTimer::GetMeasurements</a></div><div class="ttdeci">std::vector< Measurement > GetMeasurements() const override</div><div class="ttdoc">Get the recorded measurements.</div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00093">OpenClTimer.cpp:93</a></div></div> +<div class="ttc" id="a_ignore_unused_8hpp_xhtml"><div class="ttname"><a href="_ignore_unused_8hpp.xhtml">IgnoreUnused.hpp</a></div></div> +<div class="ttc" id="aclassarmnn_1_1_open_cl_timer_xhtml_adcd19a0c31e8ffa4411fa05e905c0cf4"><div class="ttname"><a href="classarmnn_1_1_open_cl_timer.xhtml#adcd19a0c31e8ffa4411fa05e905c0cf4">armnn::OpenClTimer::OpenClTimer</a></div><div class="ttdeci">OpenClTimer()</div><div class="ttdef"><b>Definition:</b> <a href="_open_cl_timer_8cpp_source.xhtml#l00017">OpenClTimer.cpp:17</a></div></div> <!-- start footer part --> <div id="nav-path" class="navpath"><!-- id is needed for treeview function! --> <ul> <li class="navelem"><a class="el" href="dir_68267d1309a1af8e8297ef4c3efbcdba.xhtml">src</a></li><li class="navelem"><a class="el" href="dir_0f3cdec46afbc61a1ded8e1687c9c9a0.xhtml">backends</a></li><li class="navelem"><a class="el" href="dir_1ad86c6d39ab715a831555571b9e98a5.xhtml">cl</a></li><li class="navelem"><a class="el" href="_open_cl_timer_8cpp.xhtml">OpenClTimer.cpp</a></li> - <li class="footer">Generated on Fri Feb 24 2023 10:24:26 for ArmNN by + <li class="footer">Generated on Wed Mar 22 2023 15:53:01 for ArmNN by <a href="http://www.doxygen.org/index.html"> - <img class="footer" src="doxygen.png" alt="doxygen"/></a> 1.8.13 </li> + <img class="footer" src="doxygen.png" alt="doxygen"/></a> 1.8.17 </li> </ul> </div> </body> |