Google Git
Sign in
apache / mxnet-site / d5c5a235eef72f64ccaf224b834a20ef3287469b / . / versions / 1.9.1 / api / cpp / docs / api / packet-inl_8h_source.html
blob: 8bf8bdb799560f8034b796c476d3d63bc2576e2b [file] [log] [blame]
<!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">
<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="viewport" content="width=device-width, initial-scale=1"/>
<title>mxnet: /work/mxnet/3rdparty/mshadow/mshadow/packet-inl.h Source File</title>
<link href="tabs.css" rel="stylesheet" type="text/css"/>
<script type="text/javascript" src="jquery.js"></script>
<script type="text/javascript" src="dynsections.js"></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>
<link href="doxygen.css" rel="stylesheet" type="text/css" />
</head>
<body>
<div id="top"><!-- do not remove this div, it is closed by doxygen! -->
<div id="titlearea">
<table cellspacing="0" cellpadding="0">
<tbody>
<tr style="height: 56px;">
<td id="projectalign" style="padding-left: 0.5em;">
<div id="projectname">mxnet
</div>
</td>
</tr>
</tbody>
</table>
</div>
<!-- end header part -->
<!-- Generated by Doxygen 1.8.13 -->
<script type="text/javascript">
var searchBox = new SearchBox("searchBox", "search",false,'Search');
</script>
<script type="text/javascript" src="menudata.js"></script>
<script type="text/javascript" src="menu.js"></script>
<script type="text/javascript">
$(function() {
initMenu('',true,false,'search.php','Search');
$(document).ready(function() { init_search(); });
});
</script>
<div id="main-nav"></div>
<!-- window showing the filter options -->
<div id="MSearchSelectWindow"
onmouseover="return searchBox.OnSearchSelectShow()"
onmouseout="return searchBox.OnSearchSelectHide()"
onkeydown="return searchBox.OnSearchSelectKey(event)">
</div>
<!-- iframe showing the search results (closed by default) -->
<div id="MSearchResultsWindow">
<iframe src="javascript:void(0)" frameborder="0"
name="MSearchResults" id="MSearchResults">
</iframe>
</div>
<div id="nav-path" class="navpath">
<ul>
<li class="navelem"><a class="el" href="dir_8cab8f464681f7cc51cee77e79a434cd.html">3rdparty</a></li><li class="navelem"><a class="el" href="dir_3e48ced36faa4eaa1b41f6d960bf0edb.html">mshadow</a></li><li class="navelem"><a class="el" href="dir_00b035bb2ad81894e6ad291054ea5f82.html">mshadow</a></li> </ul>
</div>
</div><!-- top -->
<div class="header">
<div class="headertitle">
<div class="title">packet-inl.h</div> </div>
</div><!--header-->
<div class="contents">
<a href="packet-inl_8h.html">Go to the documentation of this file.</a><div class="fragment"><div class="line"><a name="l00001"></a><span class="lineno"> 1</span>&#160;<span class="comment">/*</span></div><div class="line"><a name="l00002"></a><span class="lineno"> 2</span>&#160;<span class="comment"> * Licensed to the Apache Software Foundation (ASF) under one</span></div><div class="line"><a name="l00003"></a><span class="lineno"> 3</span>&#160;<span class="comment"> * or more contributor license agreements. See the NOTICE file</span></div><div class="line"><a name="l00004"></a><span class="lineno"> 4</span>&#160;<span class="comment"> * distributed with this work for additional information</span></div><div class="line"><a name="l00005"></a><span class="lineno"> 5</span>&#160;<span class="comment"> * regarding copyright ownership. The ASF licenses this file</span></div><div class="line"><a name="l00006"></a><span class="lineno"> 6</span>&#160;<span class="comment"> * to you under the Apache License, Version 2.0 (the</span></div><div class="line"><a name="l00007"></a><span class="lineno"> 7</span>&#160;<span class="comment"> * &quot;License&quot;); you may not use this file except in compliance</span></div><div class="line"><a name="l00008"></a><span class="lineno"> 8</span>&#160;<span class="comment"> * with the License. You may obtain a copy of the License at</span></div><div class="line"><a name="l00009"></a><span class="lineno"> 9</span>&#160;<span class="comment"> *</span></div><div class="line"><a name="l00010"></a><span class="lineno"> 10</span>&#160;<span class="comment"> * http://www.apache.org/licenses/LICENSE-2.0</span></div><div class="line"><a name="l00011"></a><span class="lineno"> 11</span>&#160;<span class="comment"> *</span></div><div class="line"><a name="l00012"></a><span class="lineno"> 12</span>&#160;<span class="comment"> * Unless required by applicable law or agreed to in writing,</span></div><div class="line"><a name="l00013"></a><span class="lineno"> 13</span>&#160;<span class="comment"> * software distributed under the License is distributed on an</span></div><div class="line"><a name="l00014"></a><span class="lineno"> 14</span>&#160;<span class="comment"> * &quot;AS IS&quot; BASIS, WITHOUT WARRANTIES OR CONDITIONS OF ANY</span></div><div class="line"><a name="l00015"></a><span class="lineno"> 15</span>&#160;<span class="comment"> * KIND, either express or implied. See the License for the</span></div><div class="line"><a name="l00016"></a><span class="lineno"> 16</span>&#160;<span class="comment"> * specific language governing permissions and limitations</span></div><div class="line"><a name="l00017"></a><span class="lineno"> 17</span>&#160;<span class="comment"> * under the License.</span></div><div class="line"><a name="l00018"></a><span class="lineno"> 18</span>&#160;<span class="comment"> */</span></div><div class="line"><a name="l00019"></a><span class="lineno"> 19</span>&#160;</div><div class="line"><a name="l00024"></a><span class="lineno"> 24</span>&#160;<span class="preprocessor">#ifndef MSHADOW_PACKET_INL_H_</span></div><div class="line"><a name="l00025"></a><span class="lineno"> 25</span>&#160;<span class="preprocessor">#define MSHADOW_PACKET_INL_H_</span></div><div class="line"><a name="l00026"></a><span class="lineno"> 26</span>&#160;</div><div class="line"><a name="l00027"></a><span class="lineno"> 27</span>&#160;<span class="preprocessor">#if defined(__APPLE__) || defined(__FreeBSD__)</span></div><div class="line"><a name="l00028"></a><span class="lineno"> 28</span>&#160;<span class="preprocessor">#include &lt;stdlib.h&gt;</span></div><div class="line"><a name="l00029"></a><span class="lineno"> 29</span>&#160;<span class="preprocessor">#else</span></div><div class="line"><a name="l00030"></a><span class="lineno"> 30</span>&#160;<span class="preprocessor">#include &lt;malloc.h&gt;</span></div><div class="line"><a name="l00031"></a><span class="lineno"> 31</span>&#160;<span class="preprocessor">#endif</span></div><div class="line"><a name="l00032"></a><span class="lineno"> 32</span>&#160;<span class="preprocessor">#include &quot;<a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html">./base.h</a>&quot;</span></div><div class="line"><a name="l00033"></a><span class="lineno"> 33</span>&#160;<span class="preprocessor">#include &quot;<a class="code" href="tensor_8h.html">./tensor.h</a>&quot;</span></div><div class="line"><a name="l00034"></a><span class="lineno"> 34</span>&#160;<span class="preprocessor">#include &quot;<a class="code" href="expression_8h.html">./expression.h</a>&quot;</span></div><div class="line"><a name="l00035"></a><span class="lineno"> 35</span>&#160;</div><div class="line"><a name="l00036"></a><span class="lineno"> 36</span>&#160;</div><div class="line"><a name="l00037"></a><span class="lineno"> 37</span>&#160;<span class="keyword">namespace </span><a class="code" href="namespacemshadow.html">mshadow</a> {</div><div class="line"><a name="l00039"></a><span class="lineno"> 39</span>&#160;<span class="keyword">namespace </span>packet {</div><div class="line"><a name="l00040"></a><span class="lineno"> 40</span>&#160;</div><div class="line"><a name="l00041"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4f"> 41</a></span>&#160;<span class="keyword">enum</span> <a class="code" href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4f">PacketArch</a> {</div><div class="line"><a name="l00042"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4fad855fb1c1aac2d1b8171f4450fb7018e"> 42</a></span>&#160; <a class="code" href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4fad855fb1c1aac2d1b8171f4450fb7018e">kPlain</a>,</div><div class="line"><a name="l00043"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4fa80fe267c1a066b1e78b8fce65a9db19e"> 43</a></span>&#160; <a class="code" href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4fa80fe267c1a066b1e78b8fce65a9db19e">kSSE2</a>,</div><div class="line"><a name="l00044"></a><span class="lineno"> 44</span>&#160;};</div><div class="line"><a name="l00045"></a><span class="lineno"> 45</span>&#160;</div><div class="line"><a name="l00046"></a><span class="lineno"> 46</span>&#160;<span class="preprocessor">#if MSHADOW_USE_SSE</span></div><div class="line"><a name="l00047"></a><span class="lineno"><a class="line" href="packet-inl_8h.html#a958737730f9e52e5d5b9cbab79ad357e"> 47</a></span>&#160;<span class="preprocessor">#define MSHADOW_DEFAULT_PACKET ::mshadow::packet::kSSE2</span></div><div class="line"><a name="l00048"></a><span class="lineno"> 48</span>&#160;<span class="preprocessor">#else</span></div><div class="line"><a name="l00049"></a><span class="lineno"> 49</span>&#160;<span class="preprocessor">#define MSHADOW_DEFAULT_PACKET ::mshadow::packet::kPlain</span></div><div class="line"><a name="l00050"></a><span class="lineno"> 50</span>&#160;<span class="preprocessor">#endif</span></div><div class="line"><a name="l00051"></a><span class="lineno"> 51</span>&#160;</div><div class="line"><a name="l00052"></a><span class="lineno"> 52</span>&#160;<span class="comment">// whether packet operator is enabled.</span></div><div class="line"><a name="l00058"></a><span class="lineno"> 58</span>&#160;<span class="comment"></span><span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch = MSHADOW_DEFAULT_PACKET&gt;</div><div class="line"><a name="l00059"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1Packet.html"> 59</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet</a>;</div><div class="line"><a name="l00060"></a><span class="lineno"> 60</span>&#160;</div><div class="line"><a name="l00061"></a><span class="lineno"> 61</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch&gt;</div><div class="line"><a name="l00062"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1AlignBytes.html"> 62</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1AlignBytes.html">AlignBytes</a> {</div><div class="line"><a name="l00063"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1AlignBytes.html#a725124e6074eb6afbfe8d32dc6335a9e"> 63</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> <a class="code" href="structmshadow_1_1packet_1_1AlignBytes.html#a725124e6074eb6afbfe8d32dc6335a9e">value</a> = 4;</div><div class="line"><a name="l00064"></a><span class="lineno"> 64</span>&#160;};</div><div class="line"><a name="l00065"></a><span class="lineno"> 65</span>&#160;</div><div class="line"><a name="l00066"></a><span class="lineno"> 66</span>&#160;} <span class="comment">// namespace packet</span></div><div class="line"><a name="l00067"></a><span class="lineno"> 67</span>&#160;} <span class="comment">// namespace mshadow</span></div><div class="line"><a name="l00068"></a><span class="lineno"> 68</span>&#160;</div><div class="line"><a name="l00069"></a><span class="lineno"> 69</span>&#160;<span class="keyword">namespace </span><a class="code" href="namespacemshadow.html">mshadow</a> {</div><div class="line"><a name="l00070"></a><span class="lineno"> 70</span>&#160;<span class="keyword">namespace </span>packet {</div><div class="line"><a name="l00077"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#ae87c3ed51219b7ae4a295884bffa5d8b"> 77</a></span>&#160;<span class="keyword">inline</span> <span class="keywordtype">void</span>* <a class="code" href="namespacemshadow_1_1packet.html#ae87c3ed51219b7ae4a295884bffa5d8b">AlignedMallocPitch</a>(<span class="keywordtype">size_t</span> *out_pitch,</div><div class="line"><a name="l00078"></a><span class="lineno"> 78</span>&#160; <span class="keywordtype">size_t</span> lspace,</div><div class="line"><a name="l00079"></a><span class="lineno"> 79</span>&#160; <span class="keywordtype">size_t</span> num_line) {</div><div class="line"><a name="l00080"></a><span class="lineno"> 80</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> bits = <a class="code" href="structmshadow_1_1packet_1_1AlignBytes.html">AlignBytes&lt;MSHADOW_DEFAULT_PACKET&gt;::value</a>;</div><div class="line"><a name="l00081"></a><span class="lineno"> 81</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> <a class="code" href="namespacemshadow_1_1expr.html#a0b4a783ea715eba66efea27dc443d9dc">mask</a> = (1 &lt;&lt; bits) - 1;</div><div class="line"><a name="l00082"></a><span class="lineno"> 82</span>&#160;</div><div class="line"><a name="l00083"></a><span class="lineno"> 83</span>&#160; <span class="keywordtype">size_t</span> pitch = ((lspace + <a class="code" href="namespacemshadow_1_1expr.html#a0b4a783ea715eba66efea27dc443d9dc">mask</a>) &gt;&gt; bits) &lt;&lt; bits;</div><div class="line"><a name="l00084"></a><span class="lineno"> 84</span>&#160; *out_pitch = pitch;</div><div class="line"><a name="l00085"></a><span class="lineno"> 85</span>&#160;<span class="preprocessor">#ifdef _MSC_VER</span></div><div class="line"><a name="l00086"></a><span class="lineno"> 86</span>&#160; <span class="keywordtype">void</span> *res = _aligned_malloc(pitch * num_line, 1 &lt;&lt; bits);</div><div class="line"><a name="l00087"></a><span class="lineno"> 87</span>&#160;<span class="preprocessor">#else</span></div><div class="line"><a name="l00088"></a><span class="lineno"> 88</span>&#160; <span class="keywordtype">void</span> *res;</div><div class="line"><a name="l00089"></a><span class="lineno"> 89</span>&#160; <span class="keywordtype">int</span> ret = posix_memalign(&amp;res, 1 &lt;&lt; bits, pitch * num_line);</div><div class="line"><a name="l00090"></a><span class="lineno"> 90</span>&#160; CHECK_EQ(ret, 0) &lt;&lt; <span class="stringliteral">&quot;AlignedMallocPitch failed&quot;</span>;</div><div class="line"><a name="l00091"></a><span class="lineno"> 91</span>&#160;<span class="preprocessor">#endif</span></div><div class="line"><a name="l00092"></a><span class="lineno"> 92</span>&#160; <span class="keywordflow">if</span> (res == NULL) {</div><div class="line"><a name="l00093"></a><span class="lineno"> 93</span>&#160; LOG(FATAL) &lt;&lt; <span class="stringliteral">&quot;AlignedMallocPitch failed&quot;</span>;</div><div class="line"><a name="l00094"></a><span class="lineno"> 94</span>&#160; }</div><div class="line"><a name="l00095"></a><span class="lineno"> 95</span>&#160;<span class="preprocessor">#if __GNUC__ &gt;= 6</span></div><div class="line"><a name="l00096"></a><span class="lineno"> 96</span>&#160;<span class="preprocessor">#pragma GCC diagnostic ignored &quot;-Wmaybe-uninitialized&quot;</span></div><div class="line"><a name="l00097"></a><span class="lineno"> 97</span>&#160;<span class="preprocessor">#endif</span></div><div class="line"><a name="l00098"></a><span class="lineno"> 98</span>&#160; <span class="keywordflow">return</span> res;</div><div class="line"><a name="l00099"></a><span class="lineno"> 99</span>&#160;<span class="preprocessor">#pragma GCC diagnostic pop</span></div><div class="line"><a name="l00100"></a><span class="lineno"> 100</span>&#160;}</div><div class="line"><a name="l00101"></a><span class="lineno"> 101</span>&#160;</div><div class="line"><a name="l00106"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#ac5a6a9a133e5c212531dbae80484c1cc"> 106</a></span>&#160;<span class="keyword">inline</span> <span class="keywordtype">void</span> <a class="code" href="namespacemshadow_1_1packet.html#ac5a6a9a133e5c212531dbae80484c1cc">AlignedFree</a>(<span class="keywordtype">void</span> *ptr) {</div><div class="line"><a name="l00107"></a><span class="lineno"> 107</span>&#160;<span class="preprocessor">#ifdef _MSC_VER</span></div><div class="line"><a name="l00108"></a><span class="lineno"> 108</span>&#160; _aligned_free(ptr);</div><div class="line"><a name="l00109"></a><span class="lineno"> 109</span>&#160;<span class="preprocessor">#else</span></div><div class="line"><a name="l00110"></a><span class="lineno"> 110</span>&#160; free(ptr);</div><div class="line"><a name="l00111"></a><span class="lineno"> 111</span>&#160;<span class="preprocessor">#endif</span></div><div class="line"><a name="l00112"></a><span class="lineno"> 112</span>&#160;}</div><div class="line"><a name="l00113"></a><span class="lineno"> 113</span>&#160;</div><div class="line"><a name="l00115"></a><span class="lineno"> 115</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch&gt;</div><div class="line"><a name="l00116"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#a60f184b1173bb7f18db29856ba1b5107"> 116</a></span>&#160;<span class="keyword">inline</span> <span class="keywordtype">bool</span> <a class="code" href="namespacemshadow_1_1packet.html#a60f184b1173bb7f18db29856ba1b5107">CheckAlign</a>(<span class="keywordtype">size_t</span> pitch) {</div><div class="line"><a name="l00117"></a><span class="lineno"> 117</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> bits = <a class="code" href="structmshadow_1_1packet_1_1AlignBytes.html">AlignBytes&lt;Arch&gt;::value</a>;</div><div class="line"><a name="l00118"></a><span class="lineno"> 118</span>&#160; <span class="keywordflow">return</span> !(pitch &amp; ((1 &lt;&lt; bits) - 1));</div><div class="line"><a name="l00119"></a><span class="lineno"> 119</span>&#160;}</div><div class="line"><a name="l00120"></a><span class="lineno"> 120</span>&#160;</div><div class="line"><a name="l00122"></a><span class="lineno"> 122</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch&gt;</div><div class="line"><a name="l00123"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#a56c210692a91896f00427c9c9d9434e9"> 123</a></span>&#160;<span class="keyword">inline</span> <span class="keywordtype">bool</span> <a class="code" href="namespacemshadow_1_1packet.html#a60f184b1173bb7f18db29856ba1b5107">CheckAlign</a>(<span class="keywordtype">void</span> *ptr) {</div><div class="line"><a name="l00124"></a><span class="lineno"> 124</span>&#160; <span class="keywordflow">return</span> CheckAlign&lt;Arch&gt;(<span class="keyword">reinterpret_cast&lt;</span><span class="keywordtype">size_t</span><span class="keyword">&gt;</span>(ptr));</div><div class="line"><a name="l00125"></a><span class="lineno"> 125</span>&#160;}</div><div class="line"><a name="l00126"></a><span class="lineno"> 126</span>&#160;</div><div class="line"><a name="l00132"></a><span class="lineno"> 132</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00133"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#a3673b9721702cf91bb412810357417a7"> 133</a></span>&#160;<span class="keyword">inline</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> <a class="code" href="namespacemshadow_1_1packet.html#a3673b9721702cf91bb412810357417a7">UpperAlign</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> size) {</div><div class="line"><a name="l00134"></a><span class="lineno"> 134</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> bits = <a class="code" href="structmshadow_1_1packet_1_1AlignBytes.html">AlignBytes&lt;MSHADOW_DEFAULT_PACKET&gt;::value</a>;</div><div class="line"><a name="l00135"></a><span class="lineno"> 135</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> <a class="code" href="namespacemshadow_1_1expr.html#a0b4a783ea715eba66efea27dc443d9dc">mask</a> = (1 &lt;&lt; bits) - 1;</div><div class="line"><a name="l00136"></a><span class="lineno"> 136</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> fsize = <span class="keyword">sizeof</span>(DType);</div><div class="line"><a name="l00137"></a><span class="lineno"> 137</span>&#160; <span class="keywordflow">return</span> (((size * fsize + mask) &gt;&gt; bits) &lt;&lt; bits) / fsize;</div><div class="line"><a name="l00138"></a><span class="lineno"> 138</span>&#160;}</div><div class="line"><a name="l00139"></a><span class="lineno"> 139</span>&#160;</div><div class="line"><a name="l00145"></a><span class="lineno"> 145</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00146"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1packet.html#aae366b300131f5212f480e9602ea232e"> 146</a></span>&#160;<span class="keyword">inline</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> <a class="code" href="namespacemshadow_1_1packet.html#aae366b300131f5212f480e9602ea232e">LowerAlign</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> size) {</div><div class="line"><a name="l00147"></a><span class="lineno"> 147</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> bits = <a class="code" href="structmshadow_1_1packet_1_1AlignBytes.html">AlignBytes&lt;MSHADOW_DEFAULT_PACKET&gt;::value</a>;</div><div class="line"><a name="l00148"></a><span class="lineno"> 148</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> fsize = <span class="keyword">sizeof</span>(DType);</div><div class="line"><a name="l00149"></a><span class="lineno"> 149</span>&#160; <span class="keywordflow">return</span> (((size * fsize) &gt;&gt; bits) &lt;&lt; bits) / fsize;</div><div class="line"><a name="l00150"></a><span class="lineno"> 150</span>&#160;}</div><div class="line"><a name="l00151"></a><span class="lineno"> 151</span>&#160;</div><div class="line"><a name="l00158"></a><span class="lineno"> 158</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> OP, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00159"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp.html"> 159</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">PacketOp</a> {</div><div class="line"><a name="l00160"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp.html#a4a55a0165215b016b70d8b8f25420eed"> 160</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kEnabled = <span class="keyword">false</span>;</div><div class="line"><a name="l00161"></a><span class="lineno"> 161</span>&#160;};</div><div class="line"><a name="l00162"></a><span class="lineno"> 162</span>&#160;<span class="comment">// specialization of operators</span></div><div class="line"><a name="l00163"></a><span class="lineno"> 163</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00164"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1plus_00_01DType_00_01Arch_01_4.html"> 164</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">PacketOp</a>&lt;op::plus, DType, Arch&gt; {</div><div class="line"><a name="l00165"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1plus_00_01DType_00_01Arch_01_4.html#acdcb8090c221f33340764a29a37f6dd6"> 165</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kEnabled = <span class="keyword">true</span>;</div><div class="line"><a name="l00166"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1plus_00_01DType_00_01Arch_01_4.html#a0bec3da978e42d7e14e3c0dd10265bfe"> 166</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <span class="keyword">static</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a> <a class="code" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1plus_00_01DType_00_01Arch_01_4.html#a0bec3da978e42d7e14e3c0dd10265bfe">Map</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; lhs,</div><div class="line"><a name="l00167"></a><span class="lineno"> 167</span>&#160; <span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; rhs) {</div><div class="line"><a name="l00168"></a><span class="lineno"> 168</span>&#160; <span class="keywordflow">return</span> lhs + rhs;</div><div class="line"><a name="l00169"></a><span class="lineno"> 169</span>&#160; }</div><div class="line"><a name="l00170"></a><span class="lineno"> 170</span>&#160;};</div><div class="line"><a name="l00171"></a><span class="lineno"> 171</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00172"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1minus_00_01DType_00_01Arch_01_4.html"> 172</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">PacketOp</a>&lt;op::minus, DType, Arch&gt; {</div><div class="line"><a name="l00173"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1minus_00_01DType_00_01Arch_01_4.html#a4cd06ab418063af4f808cc404c700352"> 173</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kEnabled = <span class="keyword">true</span>;</div><div class="line"><a name="l00174"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1minus_00_01DType_00_01Arch_01_4.html#acd57bd12afecaa17569fc7e49f47e529"> 174</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <span class="keyword">static</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a> <a class="code" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1minus_00_01DType_00_01Arch_01_4.html#acd57bd12afecaa17569fc7e49f47e529">Map</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; lhs,</div><div class="line"><a name="l00175"></a><span class="lineno"> 175</span>&#160; <span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; rhs) {</div><div class="line"><a name="l00176"></a><span class="lineno"> 176</span>&#160; <span class="keywordflow">return</span> lhs - rhs;</div><div class="line"><a name="l00177"></a><span class="lineno"> 177</span>&#160; }</div><div class="line"><a name="l00178"></a><span class="lineno"> 178</span>&#160;};</div><div class="line"><a name="l00179"></a><span class="lineno"> 179</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00180"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1mul_00_01DType_00_01Arch_01_4.html"> 180</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">PacketOp</a>&lt;op::mul, DType, Arch&gt; {</div><div class="line"><a name="l00181"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1mul_00_01DType_00_01Arch_01_4.html#a8182fafb2fed24a8fe2a45bb55c180a6"> 181</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kEnabled = <span class="keyword">true</span>;</div><div class="line"><a name="l00182"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1mul_00_01DType_00_01Arch_01_4.html#abe5dd5265fb32b4982d4457987ba31c1"> 182</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <span class="keyword">static</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a> <a class="code" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1mul_00_01DType_00_01Arch_01_4.html#abe5dd5265fb32b4982d4457987ba31c1">Map</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; lhs,</div><div class="line"><a name="l00183"></a><span class="lineno"> 183</span>&#160; <span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; rhs) {</div><div class="line"><a name="l00184"></a><span class="lineno"> 184</span>&#160; <span class="keywordflow">return</span> lhs * rhs;</div><div class="line"><a name="l00185"></a><span class="lineno"> 185</span>&#160; }</div><div class="line"><a name="l00186"></a><span class="lineno"> 186</span>&#160;};</div><div class="line"><a name="l00187"></a><span class="lineno"> 187</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00188"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1div_00_01DType_00_01Arch_01_4.html"> 188</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">PacketOp</a>&lt;op::div, DType, Arch&gt; {</div><div class="line"><a name="l00189"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1div_00_01DType_00_01Arch_01_4.html#a5ecb90abb2cef7b9754143e46e13bbc5"> 189</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kEnabled = <span class="keyword">true</span>;</div><div class="line"><a name="l00190"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1div_00_01DType_00_01Arch_01_4.html#a14b520866a99aa2cf1c9373852ca6f34"> 190</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <span class="keyword">static</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a> <a class="code" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1div_00_01DType_00_01Arch_01_4.html#a14b520866a99aa2cf1c9373852ca6f34">Map</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; lhs,</div><div class="line"><a name="l00191"></a><span class="lineno"> 191</span>&#160; <span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; rhs) {</div><div class="line"><a name="l00192"></a><span class="lineno"> 192</span>&#160; <span class="keywordflow">return</span> lhs / rhs;</div><div class="line"><a name="l00193"></a><span class="lineno"> 193</span>&#160; }</div><div class="line"><a name="l00194"></a><span class="lineno"> 194</span>&#160;};</div><div class="line"><a name="l00195"></a><span class="lineno"> 195</span>&#160;</div><div class="line"><a name="l00196"></a><span class="lineno"> 196</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00197"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1identity_00_01DType_00_01Arch_01_4.html"> 197</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">PacketOp</a>&lt;op::identity, DType, Arch&gt; {</div><div class="line"><a name="l00198"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1identity_00_01DType_00_01Arch_01_4.html#a1808efd926f39992e2b14e9c54b7f1f5"> 198</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kEnabled = <span class="keyword">true</span>;</div><div class="line"><a name="l00199"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1identity_00_01DType_00_01Arch_01_4.html#ad8fa7277ea33a870ba3285334dd204c0"> 199</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <span class="keyword">static</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a> <a class="code" href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1identity_00_01DType_00_01Arch_01_4.html#ad8fa7277ea33a870ba3285334dd204c0">Map</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;DType, Arch&gt;</a>&amp; src) {</div><div class="line"><a name="l00200"></a><span class="lineno"> 200</span>&#160; <span class="keywordflow">return</span> src;</div><div class="line"><a name="l00201"></a><span class="lineno"> 201</span>&#160; }</div><div class="line"><a name="l00202"></a><span class="lineno"> 202</span>&#160;};</div><div class="line"><a name="l00203"></a><span class="lineno"> 203</span>&#160;</div><div class="line"><a name="l00204"></a><span class="lineno"> 204</span>&#160;</div><div class="line"><a name="l00205"></a><span class="lineno"> 205</span>&#160;<span class="comment">// savers to do storage</span></div><div class="line"><a name="l00206"></a><span class="lineno"> 206</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> SV, <span class="keyword">typename</span> TFloat, PacketArch Arch&gt;</div><div class="line"><a name="l00207"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1Saver.html"> 207</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1Saver.html">Saver</a>{</div><div class="line"><a name="l00208"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1Saver.html#a7dec82ec976e778f52332accf5332109"> 208</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <span class="keyword">static</span> <span class="keywordtype">void</span> <a class="code" href="structmshadow_1_1packet_1_1Saver.html#a7dec82ec976e778f52332accf5332109">Save</a>(TFloat *dst, <span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;TFloat, Arch&gt;</a>&amp; src) {</div><div class="line"><a name="l00209"></a><span class="lineno"> 209</span>&#160; <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;TFloat, Arch&gt;</a> lhs = <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;TFloat, Arch&gt;::Load</a>(dst);</div><div class="line"><a name="l00210"></a><span class="lineno"> 210</span>&#160; <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;TFloat, Arch&gt;</a> ans = <a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">PacketOp&lt;typename SV::OPType, TFloat, Arch&gt;::Map</a>(lhs, src);</div><div class="line"><a name="l00211"></a><span class="lineno"> 211</span>&#160; ans.Store(dst);</div><div class="line"><a name="l00212"></a><span class="lineno"> 212</span>&#160; }</div><div class="line"><a name="l00213"></a><span class="lineno"> 213</span>&#160;};</div><div class="line"><a name="l00214"></a><span class="lineno"> 214</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> TFloat, PacketArch Arch&gt;</div><div class="line"><a name="l00215"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1Saver_3_01sv_1_1saveto_00_01TFloat_00_01Arch_01_4.html"> 215</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1packet_1_1Saver.html">Saver</a>&lt;sv::saveto, TFloat, Arch&gt; {</div><div class="line"><a name="l00216"></a><span class="lineno"><a class="line" href="structmshadow_1_1packet_1_1Saver_3_01sv_1_1saveto_00_01TFloat_00_01Arch_01_4.html#a84e7afff8d944df0d90a35a5057f411a"> 216</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <span class="keyword">static</span> <span class="keywordtype">void</span> <a class="code" href="structmshadow_1_1packet_1_1Saver_3_01sv_1_1saveto_00_01TFloat_00_01Arch_01_4.html#a84e7afff8d944df0d90a35a5057f411a">Save</a>(TFloat *dst, <span class="keyword">const</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">Packet&lt;TFloat, Arch&gt;</a>&amp; src) {</div><div class="line"><a name="l00217"></a><span class="lineno"> 217</span>&#160; src.Store(dst);</div><div class="line"><a name="l00218"></a><span class="lineno"> 218</span>&#160; }</div><div class="line"><a name="l00219"></a><span class="lineno"> 219</span>&#160;};</div><div class="line"><a name="l00220"></a><span class="lineno"> 220</span>&#160;} <span class="comment">// namespace packet</span></div><div class="line"><a name="l00221"></a><span class="lineno"> 221</span>&#160;} <span class="comment">// namespace mshadow</span></div><div class="line"><a name="l00222"></a><span class="lineno"> 222</span>&#160;</div><div class="line"><a name="l00223"></a><span class="lineno"> 223</span>&#160;<span class="preprocessor">#include &quot;<a class="code" href="plain-inl_8h.html">packet/plain-inl.h</a>&quot;</span></div><div class="line"><a name="l00224"></a><span class="lineno"> 224</span>&#160;<span class="preprocessor">#if MSHADOW_USE_SSE &amp;&amp; !defined(__CUDACC__)</span></div><div class="line"><a name="l00225"></a><span class="lineno"> 225</span>&#160;<span class="preprocessor">#include &quot;<a class="code" href="sse-inl_8h.html">packet/sse-inl.h</a>&quot;</span></div><div class="line"><a name="l00226"></a><span class="lineno"> 226</span>&#160;<span class="preprocessor">#endif</span></div><div class="line"><a name="l00227"></a><span class="lineno"> 227</span>&#160;</div><div class="line"><a name="l00228"></a><span class="lineno"> 228</span>&#160;<span class="keyword">namespace </span><a class="code" href="namespacemshadow.html">mshadow</a> {</div><div class="line"><a name="l00229"></a><span class="lineno"> 229</span>&#160;<span class="keyword">namespace </span>expr {</div><div class="line"><a name="l00230"></a><span class="lineno"> 230</span>&#160;</div><div class="line"><a name="l00231"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1expr.html#aa68ead86d70bad4ab69608aecb852fdd"> 231</a></span>&#160;<span class="keyword">typedef</span> <a class="code" href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4f">packet::PacketArch</a> <a class="code" href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4f">PacketArch</a>;</div><div class="line"><a name="l00232"></a><span class="lineno"> 232</span>&#160;</div><div class="line"><a name="l00233"></a><span class="lineno"> 233</span>&#160;<span class="comment">// same as plan, but use packet</span></div><div class="line"><a name="l00234"></a><span class="lineno"> 234</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> ExpType, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00235"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan.html"> 235</a></span>&#160;<span class="keyword">class </span><a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan</a> {</div><div class="line"><a name="l00236"></a><span class="lineno"> 236</span>&#160; <span class="keyword">public</span>:</div><div class="line"><a name="l00241"></a><span class="lineno"> 241</span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">packet::Packet&lt;DType, Arch&gt;</a> EvalPacket(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x) <span class="keyword">const</span>;</div><div class="line"><a name="l00242"></a><span class="lineno"> 242</span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> DType Eval(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x) <span class="keyword">const</span>;</div><div class="line"><a name="l00243"></a><span class="lineno"> 243</span>&#160;};</div><div class="line"><a name="l00244"></a><span class="lineno"> 244</span>&#160;</div><div class="line"><a name="l00245"></a><span class="lineno"> 245</span>&#160;<span class="keyword">template</span> &lt;<span class="keyword">typename</span> Device, <span class="keywordtype">int</span> dim, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00246"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html"> 246</a></span>&#160;<span class="keyword">class </span><a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan</a>&lt;<a class="code" href="structmshadow_1_1Tensor.html">Tensor</a>&lt;Device, dim, DType&gt;, DType, Arch&gt; {</div><div class="line"><a name="l00247"></a><span class="lineno"> 247</span>&#160; <span class="keyword">public</span>:</div><div class="line"><a name="l00248"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#ae7b06a333d377c584ed000b426b105cd"> 248</a></span>&#160; <span class="keyword">explicit</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#ae7b06a333d377c584ed000b426b105cd">PacketPlan</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1Tensor.html">Tensor&lt;Device, dim, DType&gt;</a> &amp;t)</div><div class="line"><a name="l00249"></a><span class="lineno"> 249</span>&#160; :dptr_(t.dptr_), stride_(t.stride_) {}</div><div class="line"><a name="l00250"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#a1252b3fd619aa1e7533077c150d8c4c3"> 250</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">packet::Packet&lt;DType, Arch&gt;</a> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#a1252b3fd619aa1e7533077c150d8c4c3">EvalPacket</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x)<span class="keyword"> const </span>{</div><div class="line"><a name="l00251"></a><span class="lineno"> 251</span>&#160; <span class="keywordflow">return</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">packet::Packet&lt;DType, Arch&gt;::Load</a>(&amp;dptr_[y * stride_ + x]);</div><div class="line"><a name="l00252"></a><span class="lineno"> 252</span>&#160; }</div><div class="line"><a name="l00253"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#afb3811e5983a4336f27fcef5673aba55"> 253</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> DType <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#afb3811e5983a4336f27fcef5673aba55">Eval</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x)<span class="keyword"> const </span>{</div><div class="line"><a name="l00254"></a><span class="lineno"> 254</span>&#160; <span class="keywordflow">return</span> dptr_[y * stride_ + x];</div><div class="line"><a name="l00255"></a><span class="lineno"> 255</span>&#160; }</div><div class="line"><a name="l00256"></a><span class="lineno"> 256</span>&#160;</div><div class="line"><a name="l00257"></a><span class="lineno"> 257</span>&#160; <span class="keyword">private</span>:</div><div class="line"><a name="l00258"></a><span class="lineno"> 258</span>&#160; <span class="keyword">const</span> DType *dptr_;</div><div class="line"><a name="l00259"></a><span class="lineno"> 259</span>&#160; <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> stride_;</div><div class="line"><a name="l00260"></a><span class="lineno"> 260</span>&#160;};</div><div class="line"><a name="l00261"></a><span class="lineno"> 261</span>&#160;</div><div class="line"><a name="l00262"></a><span class="lineno"> 262</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00263"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html"> 263</a></span>&#160;<span class="keyword">class </span><a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan</a>&lt;<a class="code" href="structmshadow_1_1expr_1_1ScalarExp.html">ScalarExp</a>&lt;DType&gt;, DType, Arch&gt; {</div><div class="line"><a name="l00264"></a><span class="lineno"> 264</span>&#160; <span class="keyword">public</span>:</div><div class="line"><a name="l00265"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a5dc48ea66a3dafff0751e2133bc8b775"> 265</a></span>&#160; <span class="keyword">explicit</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a5dc48ea66a3dafff0751e2133bc8b775">PacketPlan</a>(DType <a class="code" href="namespacemshadow_1_1expr.html#ac547eb1dceee713542019c2cc6da378b">scalar</a>) : scalar_(scalar) {}</div><div class="line"><a name="l00266"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a9a03e9d164513ab1f1ec84465a7a7ca4"> 266</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">packet::Packet&lt;DType, Arch&gt;</a> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a9a03e9d164513ab1f1ec84465a7a7ca4">EvalPacket</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x)<span class="keyword"> const </span>{</div><div class="line"><a name="l00267"></a><span class="lineno"> 267</span>&#160; <span class="keywordflow">return</span> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">packet::Packet&lt;DType, Arch&gt;::Fill</a>(scalar_);</div><div class="line"><a name="l00268"></a><span class="lineno"> 268</span>&#160; }</div><div class="line"><a name="l00269"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a9cfa748d9f3eb611d178350a72724439"> 269</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> DType <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a9cfa748d9f3eb611d178350a72724439">Eval</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x)<span class="keyword"> const </span>{</div><div class="line"><a name="l00270"></a><span class="lineno"> 270</span>&#160; <span class="keywordflow">return</span> scalar_;</div><div class="line"><a name="l00271"></a><span class="lineno"> 271</span>&#160; }</div><div class="line"><a name="l00272"></a><span class="lineno"> 272</span>&#160;</div><div class="line"><a name="l00273"></a><span class="lineno"> 273</span>&#160; <span class="keyword">private</span>:</div><div class="line"><a name="l00274"></a><span class="lineno"> 274</span>&#160; DType scalar_;</div><div class="line"><a name="l00275"></a><span class="lineno"> 275</span>&#160;};</div><div class="line"><a name="l00276"></a><span class="lineno"> 276</span>&#160;</div><div class="line"><a name="l00277"></a><span class="lineno"> 277</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keyword">typename</span> TB, <span class="keywordtype">int</span> etype, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00278"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html"> 278</a></span>&#160;<span class="keyword">class </span><a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan</a>&lt;<a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html">BinaryMapExp</a>&lt;OP, TA, TB, DType, etype&gt;, DType, Arch&gt; {</div><div class="line"><a name="l00279"></a><span class="lineno"> 279</span>&#160; <span class="keyword">public</span>:</div><div class="line"><a name="l00280"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a7408fcd2cd84bdef4ea706b6198e51a1"> 280</a></span>&#160; <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a7408fcd2cd84bdef4ea706b6198e51a1">PacketPlan</a>(<span class="keyword">const</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;TA, DType, Arch&gt;</a> &amp;lhs, <span class="keyword">const</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;TB, DType, Arch&gt;</a> &amp;rhs)</div><div class="line"><a name="l00281"></a><span class="lineno"> 281</span>&#160; : lhs_(lhs), rhs_(rhs) {}</div><div class="line"><a name="l00282"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a15cff8316690eef649844d647df4bc60"> 282</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">packet::Packet&lt;DType, Arch&gt;</a> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a15cff8316690eef649844d647df4bc60">EvalPacket</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x)<span class="keyword"> const </span>{</div><div class="line"><a name="l00283"></a><span class="lineno"> 283</span>&#160; <span class="keywordflow">return</span> <a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">packet::PacketOp&lt;OP, DType, Arch&gt;::Map</a>(lhs_.EvalPacket(y, x), rhs_.EvalPacket(y, x));</div><div class="line"><a name="l00284"></a><span class="lineno"> 284</span>&#160; }</div><div class="line"><a name="l00285"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#ac06308257244a64e6e6a6ddf7879c961"> 285</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> DType <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#ac06308257244a64e6e6a6ddf7879c961">Eval</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x)<span class="keyword"> const </span>{</div><div class="line"><a name="l00286"></a><span class="lineno"> 286</span>&#160; <span class="keywordflow">return</span> OP::Map(lhs_.Eval(y, x), rhs_.Eval(y, x));</div><div class="line"><a name="l00287"></a><span class="lineno"> 287</span>&#160; }</div><div class="line"><a name="l00288"></a><span class="lineno"> 288</span>&#160;</div><div class="line"><a name="l00289"></a><span class="lineno"> 289</span>&#160; <span class="keyword">private</span>:</div><div class="line"><a name="l00290"></a><span class="lineno"> 290</span>&#160; <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;TA, DType, Arch&gt;</a> lhs_;</div><div class="line"><a name="l00291"></a><span class="lineno"> 291</span>&#160; <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;TB, DType, Arch&gt;</a> rhs_;</div><div class="line"><a name="l00292"></a><span class="lineno"> 292</span>&#160;};</div><div class="line"><a name="l00293"></a><span class="lineno"> 293</span>&#160;</div><div class="line"><a name="l00294"></a><span class="lineno"> 294</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keywordtype">int</span> etype, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00295"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html"> 295</a></span>&#160;<span class="keyword">class </span><a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan</a>&lt;<a class="code" href="structmshadow_1_1expr_1_1UnaryMapExp.html">UnaryMapExp</a>&lt;OP, TA, DType, etype&gt;, DType, Arch&gt; {</div><div class="line"><a name="l00296"></a><span class="lineno"> 296</span>&#160; <span class="keyword">public</span>:</div><div class="line"><a name="l00297"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#ab250f3402dc64b95bcf006f828e2876d"> 297</a></span>&#160; <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#ab250f3402dc64b95bcf006f828e2876d">PacketPlan</a>(<span class="keyword">const</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;TA, DType, Arch&gt;</a> &amp;src) : src_(src) {}</div><div class="line"><a name="l00298"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a09971871cc9eb76783f035d74e1dbd2e"> 298</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> <a class="code" href="structmshadow_1_1packet_1_1Packet.html">packet::Packet&lt;DType&gt;</a> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a09971871cc9eb76783f035d74e1dbd2e">EvalPacket</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x)<span class="keyword"> const </span>{</div><div class="line"><a name="l00299"></a><span class="lineno"> 299</span>&#160; <span class="keywordflow">return</span> <a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">packet::PacketOp&lt;OP, DType, Arch&gt;::Map</a>(src_.EvalPacket(y, x));</div><div class="line"><a name="l00300"></a><span class="lineno"> 300</span>&#160; }</div><div class="line"><a name="l00301"></a><span class="lineno"><a class="line" href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a2046ac9f620cab28c31f8d89bfc4019a"> 301</a></span>&#160; <a class="code" href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a> DType <a class="code" href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a2046ac9f620cab28c31f8d89bfc4019a">Eval</a>(<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> y, <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x)<span class="keyword"> const </span>{</div><div class="line"><a name="l00302"></a><span class="lineno"> 302</span>&#160; <span class="keywordflow">return</span> OP::Map(src_.Eval(y, x));</div><div class="line"><a name="l00303"></a><span class="lineno"> 303</span>&#160; }</div><div class="line"><a name="l00304"></a><span class="lineno"> 304</span>&#160;</div><div class="line"><a name="l00305"></a><span class="lineno"> 305</span>&#160; <span class="keyword">private</span>:</div><div class="line"><a name="l00306"></a><span class="lineno"> 306</span>&#160; <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;TA, DType, Arch&gt;</a> src_;</div><div class="line"><a name="l00307"></a><span class="lineno"> 307</span>&#160;};</div><div class="line"><a name="l00308"></a><span class="lineno"> 308</span>&#160;</div><div class="line"><a name="l00309"></a><span class="lineno"> 309</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch, <span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keyword">typename</span> TB, <span class="keyword">typename</span> DType, <span class="keywordtype">int</span> etype&gt;</div><div class="line"><a name="l00310"></a><span class="lineno"> 310</span>&#160;<span class="keyword">inline</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;BinaryMapExp&lt;OP, TA, TB, DType, etype&gt;</a>, DType, Arch&gt;</div><div class="line"><a name="l00311"></a><span class="lineno"> 311</span>&#160;<a class="code" href="namespacemshadow_1_1expr.html#ac93c00afb823840232f7c369bb7c9ea6">MakePacketPlan</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html">BinaryMapExp&lt;OP, TA, TB, DType, etype&gt;</a> &amp;e);</div><div class="line"><a name="l00312"></a><span class="lineno"> 312</span>&#160;</div><div class="line"><a name="l00313"></a><span class="lineno"> 313</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch, <span class="keyword">typename</span> DType&gt;</div><div class="line"><a name="l00314"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1expr.html#a29fa0bd6d47c6e00183a22d76bcdcb91"> 314</a></span>&#160;<span class="keyword">inline</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;ScalarExp&lt;DType&gt;</a>, DType, Arch&gt; <a class="code" href="namespacemshadow_1_1expr.html#ac93c00afb823840232f7c369bb7c9ea6">MakePacketPlan</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1expr_1_1ScalarExp.html">ScalarExp&lt;DType&gt;</a> &amp;e) {</div><div class="line"><a name="l00315"></a><span class="lineno"> 315</span>&#160; <span class="keywordflow">return</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;ScalarExp&lt;DType&gt;</a>, DType, Arch&gt;(e.<a class="code" href="structmshadow_1_1expr_1_1ScalarExp.html#a8c1e8ed3c405b3fc464861a47ab13a0a">scalar_</a>);</div><div class="line"><a name="l00316"></a><span class="lineno"> 316</span>&#160;}</div><div class="line"><a name="l00317"></a><span class="lineno"> 317</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch, <span class="keyword">typename</span> T, <span class="keyword">typename</span> DType&gt;</div><div class="line"><a name="l00318"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1expr.html#a68dab94b738d83d5715c2a8f5d7fefaa"> 318</a></span>&#160;<span class="keyword">inline</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;T, DType, Arch&gt;</a> <a class="code" href="namespacemshadow_1_1expr.html#ac93c00afb823840232f7c369bb7c9ea6">MakePacketPlan</a>(<span class="keyword">const</span> <a class="code" href="classmshadow_1_1expr_1_1RValueExp.html">RValueExp&lt;T, DType&gt;</a> &amp;e) {</div><div class="line"><a name="l00319"></a><span class="lineno"> 319</span>&#160; <span class="keywordflow">return</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;T, DType, Arch&gt;</a>(e.<a class="code" href="structmshadow_1_1expr_1_1Exp.html#adb7e4afd0baed78d66cff87de0a6621f">self</a>());</div><div class="line"><a name="l00320"></a><span class="lineno"> 320</span>&#160;}</div><div class="line"><a name="l00321"></a><span class="lineno"> 321</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch, <span class="keyword">typename</span> T, <span class="keywordtype">int</span> dim, <span class="keyword">typename</span> DType&gt;</div><div class="line"><a name="l00322"></a><span class="lineno"> 322</span>&#160;<span class="keyword">inline</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;T, DType, Arch&gt;</a></div><div class="line"><a name="l00323"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1expr.html#a3aa9c46e197655eeb98fcd8ecab74114"> 323</a></span>&#160;<a class="code" href="namespacemshadow_1_1expr.html#ac93c00afb823840232f7c369bb7c9ea6">MakePacketPlan</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1expr_1_1MakeTensorExp.html">MakeTensorExp&lt;T, cpu, dim, DType&gt;</a> &amp;e) {</div><div class="line"><a name="l00324"></a><span class="lineno"> 324</span>&#160; <span class="keywordflow">return</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;T, DType, Arch&gt;</a>(e.<a class="code" href="structmshadow_1_1expr_1_1MakeTensorExp.html#adf83aad5be17b50320bfcc6430244439">real_self</a>());</div><div class="line"><a name="l00325"></a><span class="lineno"> 325</span>&#160;}</div><div class="line"><a name="l00326"></a><span class="lineno"> 326</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch, <span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keyword">typename</span> DType, <span class="keywordtype">int</span> etype&gt;</div><div class="line"><a name="l00327"></a><span class="lineno"> 327</span>&#160;<span class="keyword">inline</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">PacketPlan&lt;UnaryMapExp&lt;OP, TA, DType, etype&gt;</a>, DType, Arch&gt;</div><div class="line"><a name="l00328"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1expr.html#ac93c00afb823840232f7c369bb7c9ea6"> 328</a></span>&#160;<a class="code" href="namespacemshadow_1_1expr.html#ac93c00afb823840232f7c369bb7c9ea6">MakePacketPlan</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1expr_1_1UnaryMapExp.html">UnaryMapExp&lt;OP, TA, DType, etype&gt;</a> &amp;e) {</div><div class="line"><a name="l00329"></a><span class="lineno"> 329</span>&#160; <span class="keywordflow">return</span> PacketPlan&lt;UnaryMapExp&lt;OP, TA, DType, etype&gt;, DType, Arch&gt;(MakePacketPlan&lt;Arch&gt;(e.<a class="code" href="structmshadow_1_1expr_1_1UnaryMapExp.html#a2916051247ff9e5f1ff4c5020738d36c">src_</a>));</div><div class="line"><a name="l00330"></a><span class="lineno"> 330</span>&#160;}</div><div class="line"><a name="l00331"></a><span class="lineno"> 331</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch, <span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keyword">typename</span> TB, <span class="keyword">typename</span> DType, <span class="keywordtype">int</span> etype&gt;</div><div class="line"><a name="l00332"></a><span class="lineno"> 332</span>&#160;<span class="keyword">inline</span> PacketPlan&lt;BinaryMapExp&lt;OP, TA, TB, DType, etype&gt;, DType, Arch&gt;</div><div class="line"><a name="l00333"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1expr.html#a6637e9ac02f51c65440dc7eb719e951d"> 333</a></span>&#160;<a class="code" href="namespacemshadow_1_1expr.html#ac93c00afb823840232f7c369bb7c9ea6">MakePacketPlan</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html">BinaryMapExp&lt;OP, TA, TB, DType, etype&gt;</a> &amp;e) {</div><div class="line"><a name="l00334"></a><span class="lineno"> 334</span>&#160; <span class="keywordflow">return</span> PacketPlan&lt;BinaryMapExp&lt;OP, TA, TB, DType, etype&gt;,</div><div class="line"><a name="l00335"></a><span class="lineno"> 335</span>&#160; DType, Arch&gt;(MakePacketPlan&lt;Arch&gt;(e.<a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html#ae4d3d912e56bbad508abeeed4743c38c">lhs_</a>), MakePacketPlan&lt;Arch&gt;(e.<a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html#a9afdad54a6a226b251fc4cd4ed92050f">rhs_</a>));</div><div class="line"><a name="l00336"></a><span class="lineno"> 336</span>&#160;}</div><div class="line"><a name="l00337"></a><span class="lineno"> 337</span>&#160;</div><div class="line"><a name="l00345"></a><span class="lineno"> 345</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> E, PacketArch Arch&gt;</div><div class="line"><a name="l00346"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck.html"> 346</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck</a>{</div><div class="line"><a name="l00347"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck.html#ad1d72397187569f143e8f0328ee75aca"> 347</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kPass = <span class="keyword">false</span>;</div><div class="line"><a name="l00348"></a><span class="lineno"> 348</span>&#160;};</div><div class="line"><a name="l00349"></a><span class="lineno"> 349</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch&gt;</div><div class="line"><a name="l00350"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01float_00_01Arch_01_4.html"> 350</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck</a>&lt;float, Arch&gt; {</div><div class="line"><a name="l00351"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01float_00_01Arch_01_4.html#a5527272dd865455bfdad9aeca5fc2b92"> 351</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kPass = <span class="keyword">true</span>;</div><div class="line"><a name="l00352"></a><span class="lineno"> 352</span>&#160;};</div><div class="line"><a name="l00353"></a><span class="lineno"> 353</span>&#160;<span class="keyword">template</span>&lt;PacketArch Arch&gt;</div><div class="line"><a name="l00354"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01double_00_01Arch_01_4.html"> 354</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck</a>&lt;double, Arch&gt; {</div><div class="line"><a name="l00355"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01double_00_01Arch_01_4.html#a78256a5b44e22306c400a32cc1802cd5"> 355</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kPass = <span class="keyword">true</span>;</div><div class="line"><a name="l00356"></a><span class="lineno"> 356</span>&#160;};</div><div class="line"><a name="l00357"></a><span class="lineno"> 357</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00358"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01ScalarExp_3_01DType_01_4_00_01Arch_01_4.html"> 358</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck</a>&lt;<a class="code" href="structmshadow_1_1expr_1_1ScalarExp.html">ScalarExp</a>&lt;DType&gt;, Arch&gt; {</div><div class="line"><a name="l00359"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01ScalarExp_3_01DType_01_4_00_01Arch_01_4.html#a70410d14e86e98ba02fa23b323a95a98"> 359</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kPass = <a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck&lt;DType, Arch&gt;::kPass</a>;</div><div class="line"><a name="l00360"></a><span class="lineno"> 360</span>&#160;};</div><div class="line"><a name="l00361"></a><span class="lineno"> 361</span>&#160;<span class="keyword">template</span>&lt;<span class="keywordtype">int</span> dim, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00362"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01Tensor_3_01cpu_00_01dim_00_01DType_01_4_00_01Arch_01_4.html"> 362</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck</a>&lt;<a class="code" href="structmshadow_1_1Tensor.html">Tensor</a>&lt;<a class="code" href="structmshadow_1_1cpu.html">cpu</a>, dim, DType&gt;, Arch&gt; {</div><div class="line"><a name="l00363"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01Tensor_3_01cpu_00_01dim_00_01DType_01_4_00_01Arch_01_4.html#ad2028bda6f308bc8563e303eaed74a39"> 363</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kPass = <a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck&lt;DType, Arch&gt;::kPass</a>;</div><div class="line"><a name="l00364"></a><span class="lineno"> 364</span>&#160;};</div><div class="line"><a name="l00365"></a><span class="lineno"> 365</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keyword">typename</span> DType, <span class="keywordtype">int</span> etype, PacketArch Arch&gt;</div><div class="line"><a name="l00366"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01Arch_01_4.html"> 366</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck</a>&lt;<a class="code" href="structmshadow_1_1expr_1_1UnaryMapExp.html">UnaryMapExp</a>&lt;OP, TA, DType, etype&gt;, Arch&gt; {</div><div class="line"><a name="l00367"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01Arch_01_4.html#a40395c0d83f49e5469af47b762ae6cd9"> 367</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kPass = <a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck&lt;TA, Arch&gt;::kPass</a> &amp;&amp;</div><div class="line"><a name="l00368"></a><span class="lineno"> 368</span>&#160; <a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">packet::PacketOp&lt;OP, DType, Arch&gt;::kEnabled</a>;</div><div class="line"><a name="l00369"></a><span class="lineno"> 369</span>&#160;};</div><div class="line"><a name="l00370"></a><span class="lineno"> 370</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keyword">typename</span> TB, <span class="keyword">typename</span> DType, <span class="keywordtype">int</span> etype, PacketArch Arch&gt;</div><div class="line"><a name="l00371"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01Arch_01_4.html"> 371</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck</a>&lt; <a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html">BinaryMapExp</a>&lt;OP, TA, TB, DType, etype&gt;, Arch&gt; {</div><div class="line"><a name="l00372"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketCheck_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01Arch_01_4.html#a1194677bcf9db07b9b4c1eda922a695c"> 372</a></span>&#160; <span class="keyword">static</span> <span class="keyword">const</span> <span class="keywordtype">bool</span> kPass = <a class="code" href="structmshadow_1_1packet_1_1PacketOp.html">packet::PacketOp&lt;OP, DType, Arch&gt;::kEnabled</a> &amp;&amp;</div><div class="line"><a name="l00373"></a><span class="lineno"> 373</span>&#160; <a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck&lt;TA, Arch&gt;::kPass</a> &amp;&amp; <a class="code" href="structmshadow_1_1expr_1_1PacketCheck.html">PacketCheck&lt;TB, Arch&gt;::kPass</a>;</div><div class="line"><a name="l00374"></a><span class="lineno"> 374</span>&#160;};</div><div class="line"><a name="l00375"></a><span class="lineno"> 375</span>&#160;<span class="comment">//----------------------------------------------------</span></div><div class="line"><a name="l00376"></a><span class="lineno"> 376</span>&#160;<span class="comment">// Check if data is aligned and allow packet operation</span></div><div class="line"><a name="l00377"></a><span class="lineno"> 377</span>&#160;<span class="comment">//----------------------------------------------------</span></div><div class="line"><a name="l00378"></a><span class="lineno"> 378</span>&#160;<span class="keyword">template</span>&lt;<span class="keywordtype">int</span> dim, <span class="keyword">typename</span> E, PacketArch Arch&gt;</div><div class="line"><a name="l00379"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck.html"> 379</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html">PacketAlignCheck</a> {</div><div class="line"><a name="l00380"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck.html#acddff0d48652e427883ee17aa870acd5"> 380</a></span>&#160; <span class="keyword">inline</span> <span class="keyword">static</span> <span class="keywordtype">bool</span> <a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html#acddff0d48652e427883ee17aa870acd5">Check</a>(<span class="keyword">const</span> E &amp;exp) {</div><div class="line"><a name="l00381"></a><span class="lineno"> 381</span>&#160; <span class="keywordflow">return</span> <span class="keyword">false</span>;</div><div class="line"><a name="l00382"></a><span class="lineno"> 382</span>&#160; }</div><div class="line"><a name="l00383"></a><span class="lineno"> 383</span>&#160;};</div><div class="line"><a name="l00384"></a><span class="lineno"> 384</span>&#160;<span class="keyword">template</span>&lt;<span class="keywordtype">int</span> dim, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00385"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01ScalarExp_3_01DType_01_4_00_01Arch_01_4.html"> 385</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html">PacketAlignCheck</a>&lt;dim, <a class="code" href="structmshadow_1_1expr_1_1ScalarExp.html">ScalarExp</a>&lt;DType&gt;, Arch&gt; {</div><div class="line"><a name="l00386"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01ScalarExp_3_01DType_01_4_00_01Arch_01_4.html#a408f18d184aebd10227649a1d40a3e86"> 386</a></span>&#160; <span class="keyword">inline</span> <span class="keyword">static</span> <span class="keywordtype">bool</span> <a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01ScalarExp_3_01DType_01_4_00_01Arch_01_4.html#a408f18d184aebd10227649a1d40a3e86">Check</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1expr_1_1ScalarExp.html">ScalarExp&lt;DType&gt;</a> &amp;exp) {</div><div class="line"><a name="l00387"></a><span class="lineno"> 387</span>&#160; <span class="keywordflow">return</span> <span class="keyword">true</span>;</div><div class="line"><a name="l00388"></a><span class="lineno"> 388</span>&#160; }</div><div class="line"><a name="l00389"></a><span class="lineno"> 389</span>&#160;};</div><div class="line"><a name="l00390"></a><span class="lineno"> 390</span>&#160;<span class="keyword">template</span>&lt;<span class="keywordtype">int</span> dim, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00391"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01Tensor_3_01cpu_00_01dim_00_01DType_01_4_00_01Arch_01_4.html"> 391</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html">PacketAlignCheck</a>&lt;dim, <a class="code" href="structmshadow_1_1Tensor.html">Tensor</a>&lt;<a class="code" href="structmshadow_1_1cpu.html">cpu</a>, dim, DType&gt;, Arch&gt; {</div><div class="line"><a name="l00392"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01Tensor_3_01cpu_00_01dim_00_01DType_01_4_00_01Arch_01_4.html#af613d87cfd68b9bd4f01895dadf38014"> 392</a></span>&#160; <span class="keyword">inline</span> <span class="keyword">static</span> <span class="keywordtype">bool</span> <a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01Tensor_3_01cpu_00_01dim_00_01DType_01_4_00_01Arch_01_4.html#af613d87cfd68b9bd4f01895dadf38014">Check</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1Tensor.html">Tensor&lt;cpu, dim, DType&gt;</a> &amp;t) {</div><div class="line"><a name="l00393"></a><span class="lineno"> 393</span>&#160; <span class="keywordflow">return</span> packet::CheckAlign&lt;Arch&gt;(t.<a class="code" href="structmshadow_1_1Tensor.html#ad86d6759c585efb5229b3a0659973838">dptr_</a>) &amp;&amp;</div><div class="line"><a name="l00394"></a><span class="lineno"> 394</span>&#160; packet::CheckAlign&lt;Arch&gt;(t.<a class="code" href="structmshadow_1_1Tensor.html#afee556f188e29bbd0ecc45fe98d3c1c3">stride_</a> * <span class="keyword">sizeof</span>(DType));</div><div class="line"><a name="l00395"></a><span class="lineno"> 395</span>&#160; }</div><div class="line"><a name="l00396"></a><span class="lineno"> 396</span>&#160;};</div><div class="line"><a name="l00397"></a><span class="lineno"> 397</span>&#160;<span class="keyword">template</span>&lt;<span class="keywordtype">int</span> dim, <span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keyword">typename</span> DType, <span class="keywordtype">int</span> etype, PacketArch Arch&gt;</div><div class="line"><a name="l00398"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01Arch_01_4.html"> 398</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html">PacketAlignCheck</a>&lt;dim, <a class="code" href="structmshadow_1_1expr_1_1UnaryMapExp.html">UnaryMapExp</a>&lt;OP, TA, DType, etype&gt;, Arch&gt; {</div><div class="line"><a name="l00399"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01Arch_01_4.html#ae4fd9e0d56b69e959ace381a8c11f329"> 399</a></span>&#160; <span class="keyword">inline</span> <span class="keyword">static</span> <span class="keywordtype">bool</span> <a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01Arch_01_4.html#ae4fd9e0d56b69e959ace381a8c11f329">Check</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1expr_1_1UnaryMapExp.html">UnaryMapExp&lt;OP, TA, DType, etype&gt;</a> &amp;t) {</div><div class="line"><a name="l00400"></a><span class="lineno"> 400</span>&#160; <span class="keywordflow">return</span> <a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html">PacketAlignCheck&lt;dim, TA, Arch&gt;::Check</a>(t.<a class="code" href="structmshadow_1_1expr_1_1UnaryMapExp.html#a2916051247ff9e5f1ff4c5020738d36c">src_</a>);</div><div class="line"><a name="l00401"></a><span class="lineno"> 401</span>&#160; }</div><div class="line"><a name="l00402"></a><span class="lineno"> 402</span>&#160;};</div><div class="line"><a name="l00403"></a><span class="lineno"> 403</span>&#160;<span class="keyword">template</span>&lt;<span class="keywordtype">int</span> dim, <span class="keyword">typename</span> OP, <span class="keyword">typename</span> TA, <span class="keyword">typename</span> TB,</div><div class="line"><a name="l00404"></a><span class="lineno"> 404</span>&#160; <span class="keyword">typename</span> DType, <span class="keywordtype">int</span> etype, PacketArch Arch&gt;</div><div class="line"><a name="l00405"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01710a64b86afbf8d7faec025f10b905b0.html"> 405</a></span>&#160;<span class="keyword">struct </span><a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html">PacketAlignCheck</a>&lt;dim, <a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html">BinaryMapExp</a>&lt;OP, TA, TB, DType, etype&gt;, Arch&gt; {</div><div class="line"><a name="l00406"></a><span class="lineno"><a class="line" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01710a64b86afbf8d7faec025f10b905b0.html#acbddc0995f0dea05454823f29fac922b"> 406</a></span>&#160; <span class="keyword">inline</span> <span class="keyword">static</span> <span class="keywordtype">bool</span> <a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01710a64b86afbf8d7faec025f10b905b0.html#acbddc0995f0dea05454823f29fac922b">Check</a>(<span class="keyword">const</span> <a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html">BinaryMapExp&lt;OP, TA, TB, DType, etype&gt;</a> &amp;t) {</div><div class="line"><a name="l00407"></a><span class="lineno"> 407</span>&#160; <span class="keywordflow">return</span> <a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html">PacketAlignCheck&lt;dim, TA, Arch&gt;::Check</a>(t.<a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html#ae4d3d912e56bbad508abeeed4743c38c">lhs_</a>) &amp;&amp;</div><div class="line"><a name="l00408"></a><span class="lineno"> 408</span>&#160; <a class="code" href="structmshadow_1_1expr_1_1PacketAlignCheck.html">PacketAlignCheck&lt;dim, TB, Arch&gt;::Check</a>(t.<a class="code" href="structmshadow_1_1expr_1_1BinaryMapExp.html#a9afdad54a6a226b251fc4cd4ed92050f">rhs_</a>);</div><div class="line"><a name="l00409"></a><span class="lineno"> 409</span>&#160; }</div><div class="line"><a name="l00410"></a><span class="lineno"> 410</span>&#160;};</div><div class="line"><a name="l00411"></a><span class="lineno"> 411</span>&#160;</div><div class="line"><a name="l00415"></a><span class="lineno"> 415</span>&#160;<span class="keyword">template</span>&lt;<span class="keyword">typename</span> SV, <span class="keyword">typename</span> E, <span class="keywordtype">int</span> dim, <span class="keyword">typename</span> DType, PacketArch Arch&gt;</div><div class="line"><a name="l00416"></a><span class="lineno"><a class="line" href="namespacemshadow_1_1expr.html#a8fb88661f1972b4614493ba09934fc1b"> 416</a></span>&#160;<span class="keyword">inline</span> <span class="keywordtype">void</span> <a class="code" href="namespacemshadow_1_1expr.html#a8fb88661f1972b4614493ba09934fc1b">MapPacketPlan</a>(<a class="code" href="structmshadow_1_1Tensor.html">Tensor&lt;cpu, dim, DType&gt;</a> _dst,</div><div class="line"><a name="l00417"></a><span class="lineno"> 417</span>&#160; <span class="keyword">const</span> <a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html">expr::PacketPlan&lt;E, DType, Arch&gt;</a>&amp; plan) {</div><div class="line"><a name="l00418"></a><span class="lineno"> 418</span>&#160; <a class="code" href="structmshadow_1_1Tensor.html">Tensor&lt;cpu, 2, DType&gt;</a> dst = _dst.<a class="code" href="structmshadow_1_1Tensor.html#a48a5927e810fbc45e43e92cfe397d9f2">FlatTo2D</a>();</div><div class="line"><a name="l00419"></a><span class="lineno"> 419</span>&#160; <span class="keyword">const</span> <a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> xlen = packet::LowerAlign&lt;DType, Arch&gt;(dst.<a class="code" href="structmshadow_1_1Tensor.html#a88cbcae11653307bfa4c99804320b638">size</a>(1));</div><div class="line"><a name="l00420"></a><span class="lineno"> 420</span>&#160; <span class="keyword">const</span> <span class="keywordtype">size_t</span> packetSize = <a class="code" href="structmshadow_1_1packet_1_1Packet.html">packet::Packet&lt;DType, Arch&gt;::size</a>;</div><div class="line"><a name="l00421"></a><span class="lineno"> 421</span>&#160;<span class="preprocessor">#ifndef __CUDACC__</span></div><div class="line"><a name="l00422"></a><span class="lineno"> 422</span>&#160;<span class="preprocessor"> #pragma omp parallel for</span></div><div class="line"><a name="l00423"></a><span class="lineno"> 423</span>&#160;<span class="preprocessor">#endif</span></div><div class="line"><a name="l00424"></a><span class="lineno"> 424</span>&#160; <span class="keywordflow">for</span> (<a class="code" href="namespacemshadow.html#aa94c153a2f8bcd10be82a4f5598ae5b9">openmp_index_t</a> y = 0; y &lt; dst.<a class="code" href="structmshadow_1_1Tensor.html#a88cbcae11653307bfa4c99804320b638">size</a>(0); ++y) {</div><div class="line"><a name="l00425"></a><span class="lineno"> 425</span>&#160; <span class="keywordflow">for</span> (<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x = 0; x &lt; xlen; x += packetSize) {</div><div class="line"><a name="l00426"></a><span class="lineno"> 426</span>&#160; <a class="code" href="structmshadow_1_1packet_1_1Saver.html#a7dec82ec976e778f52332accf5332109">packet::Saver&lt;SV, DType, Arch&gt;::Save</a>(&amp;dst[y][x], plan.<a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html#a9f13cc90187ac190d0e336c6b9cd20a3">EvalPacket</a>(y, x));</div><div class="line"><a name="l00427"></a><span class="lineno"> 427</span>&#160; }</div><div class="line"><a name="l00428"></a><span class="lineno"> 428</span>&#160; <span class="keywordflow">for</span> (<a class="code" href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">index_t</a> x = xlen; x &lt; dst.<a class="code" href="structmshadow_1_1Tensor.html#a88cbcae11653307bfa4c99804320b638">size</a>(1); ++x) {</div><div class="line"><a name="l00429"></a><span class="lineno"> 429</span>&#160; SV::Save(dst[y][x], plan.<a class="code" href="classmshadow_1_1expr_1_1PacketPlan.html#a020eee5397c1126cd1ae354bb8b59149">Eval</a>(y, x));</div><div class="line"><a name="l00430"></a><span class="lineno"> 430</span>&#160; }</div><div class="line"><a name="l00431"></a><span class="lineno"> 431</span>&#160; }</div><div class="line"><a name="l00432"></a><span class="lineno"> 432</span>&#160;}</div><div class="line"><a name="l00433"></a><span class="lineno"> 433</span>&#160;} <span class="comment">// namespace expr</span></div><div class="line"><a name="l00434"></a><span class="lineno"> 434</span>&#160;} <span class="comment">// namespace mshadow</span></div><div class="line"><a name="l00435"></a><span class="lineno"> 435</span>&#160;<span class="preprocessor">#endif // MSHADOW_PACKET_INL_H_</span></div><div class="ttc" id="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1div_00_01DType_00_01Arch_01_4_html_a14b520866a99aa2cf1c9373852ca6f34"><div class="ttname"><a href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1div_00_01DType_00_01Arch_01_4.html#a14b520866a99aa2cf1c9373852ca6f34">mshadow::packet::PacketOp&lt; op::div, DType, Arch &gt;::Map</a></div><div class="ttdeci">static MSHADOW_CINLINE Packet&lt; DType, Arch &gt; Map(const Packet&lt; DType, Arch &gt; &amp;lhs, const Packet&lt; DType, Arch &gt; &amp;rhs)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:190</div></div>
<div class="ttc" id="namespacemshadow_1_1expr_html_ac547eb1dceee713542019c2cc6da378b"><div class="ttname"><a href="namespacemshadow_1_1expr.html#ac547eb1dceee713542019c2cc6da378b">mshadow::expr::scalar</a></div><div class="ttdeci">ScalarExp&lt; DType &gt; scalar(DType s)</div><div class="ttdoc">create an scalar expression </div><div class="ttdef"><b>Definition:</b> expression.h:103</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_html"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan.html">mshadow::expr::PacketPlan</a></div><div class="ttdef"><b>Definition:</b> packet-inl.h:235</div></div>
<div class="ttc" id="structmshadow_1_1Tensor_html_ad86d6759c585efb5229b3a0659973838"><div class="ttname"><a href="structmshadow_1_1Tensor.html#ad86d6759c585efb5229b3a0659973838">mshadow::Tensor::dptr_</a></div><div class="ttdeci">DType * dptr_</div><div class="ttdoc">pointer to the data </div><div class="ttdef"><b>Definition:</b> tensor.h:434</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1Exp_html_adb7e4afd0baed78d66cff87de0a6621f"><div class="ttname"><a href="structmshadow_1_1expr_1_1Exp.html#adb7e4afd0baed78d66cff87de0a6621f">mshadow::expr::Exp&lt; Container, DType, type::kRValue &gt;::self</a></div><div class="ttdeci">const Container &amp; self(void) const</div><div class="ttdef"><b>Definition:</b> expression.h:82</div></div>
<div class="ttc" id="namespacemshadow_1_1packet_html_ac5a6a9a133e5c212531dbae80484c1cc"><div class="ttname"><a href="namespacemshadow_1_1packet.html#ac5a6a9a133e5c212531dbae80484c1cc">mshadow::packet::AlignedFree</a></div><div class="ttdeci">void AlignedFree(void *ptr)</div><div class="ttdoc">free aligned space </div><div class="ttdef"><b>Definition:</b> packet-inl.h:106</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1BinaryMapExp_html_a9afdad54a6a226b251fc4cd4ed92050f"><div class="ttname"><a href="structmshadow_1_1expr_1_1BinaryMapExp.html#a9afdad54a6a226b251fc4cd4ed92050f">mshadow::expr::BinaryMapExp::rhs_</a></div><div class="ttdeci">const TB &amp; rhs_</div><div class="ttdoc">right operand </div><div class="ttdef"><b>Definition:</b> expression.h:339</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4_html_ac06308257244a64e6e6a6ddf7879c961"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#ac06308257244a64e6e6a6ddf7879c961">mshadow::expr::PacketPlan&lt; BinaryMapExp&lt; OP, TA, TB, DType, etype &gt;, DType, Arch &gt;::Eval</a></div><div class="ttdeci">MSHADOW_CINLINE DType Eval(index_t y, index_t x) const</div><div class="ttdef"><b>Definition:</b> packet-inl.h:285</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1PacketAlignCheck_html"><div class="ttname"><a href="structmshadow_1_1expr_1_1PacketAlignCheck.html">mshadow::expr::PacketAlignCheck</a></div><div class="ttdef"><b>Definition:</b> packet-inl.h:379</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4_html_a2046ac9f620cab28c31f8d89bfc4019a"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a2046ac9f620cab28c31f8d89bfc4019a">mshadow::expr::PacketPlan&lt; UnaryMapExp&lt; OP, TA, DType, etype &gt;, DType, Arch &gt;::Eval</a></div><div class="ttdeci">MSHADOW_CINLINE DType Eval(index_t y, index_t x) const</div><div class="ttdef"><b>Definition:</b> packet-inl.h:301</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1PacketAlignCheck_html_acddff0d48652e427883ee17aa870acd5"><div class="ttname"><a href="structmshadow_1_1expr_1_1PacketAlignCheck.html#acddff0d48652e427883ee17aa870acd5">mshadow::expr::PacketAlignCheck::Check</a></div><div class="ttdeci">static bool Check(const E &amp;exp)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:380</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1BinaryMapExp_html"><div class="ttname"><a href="structmshadow_1_1expr_1_1BinaryMapExp.html">mshadow::expr::BinaryMapExp</a></div><div class="ttdoc">binary map expression lhs [op] rhs </div><div class="ttdef"><b>Definition:</b> expression.h:334</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1AlignBytes_html_a725124e6074eb6afbfe8d32dc6335a9e"><div class="ttname"><a href="structmshadow_1_1packet_1_1AlignBytes.html#a725124e6074eb6afbfe8d32dc6335a9e">mshadow::packet::AlignBytes::value</a></div><div class="ttdeci">static const index_t value</div><div class="ttdef"><b>Definition:</b> packet-inl.h:63</div></div>
<div class="ttc" id="namespacemshadow_1_1expr_html_ac93c00afb823840232f7c369bb7c9ea6"><div class="ttname"><a href="namespacemshadow_1_1expr.html#ac93c00afb823840232f7c369bb7c9ea6">mshadow::expr::MakePacketPlan</a></div><div class="ttdeci">PacketPlan&lt; UnaryMapExp&lt; OP, TA, DType, etype &gt;, DType, Arch &gt; MakePacketPlan(const UnaryMapExp&lt; OP, TA, DType, etype &gt; &amp;e)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:328</div></div>
<div class="ttc" id="namespacemshadow_1_1packet_html_ae87c3ed51219b7ae4a295884bffa5d8b"><div class="ttname"><a href="namespacemshadow_1_1packet.html#ae87c3ed51219b7ae4a295884bffa5d8b">mshadow::packet::AlignedMallocPitch</a></div><div class="ttdeci">void * AlignedMallocPitch(size_t *out_pitch, size_t lspace, size_t num_line)</div><div class="ttdoc">analog to cudaMallocPitch, allocate a aligned space with num_line * lspace cells </div><div class="ttdef"><b>Definition:</b> packet-inl.h:77</div></div>
<div class="ttc" id="namespacemshadow_1_1packet_html_a69941771d29a1ae9a744c3e6c8b4ab4fad855fb1c1aac2d1b8171f4450fb7018e"><div class="ttname"><a href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4fad855fb1c1aac2d1b8171f4450fb7018e">mshadow::packet::kPlain</a></div><div class="ttdef"><b>Definition:</b> packet-inl.h:42</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1RValueExp_html"><div class="ttname"><a href="classmshadow_1_1expr_1_1RValueExp.html">mshadow::expr::RValueExp</a></div><div class="ttdoc">base class of all rvalues </div><div class="ttdef"><b>Definition:</b> expression.h:148</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1ScalarExp_html_a8c1e8ed3c405b3fc464861a47ab13a0a"><div class="ttname"><a href="structmshadow_1_1expr_1_1ScalarExp.html#a8c1e8ed3c405b3fc464861a47ab13a0a">mshadow::expr::ScalarExp::scalar_</a></div><div class="ttdeci">DType scalar_</div><div class="ttdoc">scalar value </div><div class="ttdef"><b>Definition:</b> expression.h:97</div></div>
<div class="ttc" id="namespacemshadow_1_1packet_html_a69941771d29a1ae9a744c3e6c8b4ab4f"><div class="ttname"><a href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4f">mshadow::packet::PacketArch</a></div><div class="ttdeci">PacketArch</div><div class="ttdef"><b>Definition:</b> packet-inl.h:41</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4_html_a7408fcd2cd84bdef4ea706b6198e51a1"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a7408fcd2cd84bdef4ea706b6198e51a1">mshadow::expr::PacketPlan&lt; BinaryMapExp&lt; OP, TA, TB, DType, etype &gt;, DType, Arch &gt;::PacketPlan</a></div><div class="ttdeci">PacketPlan(const PacketPlan&lt; TA, DType, Arch &gt; &amp;lhs, const PacketPlan&lt; TB, DType, Arch &gt; &amp;rhs)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:280</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1identity_00_01DType_00_01Arch_01_4_html_ad8fa7277ea33a870ba3285334dd204c0"><div class="ttname"><a href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1identity_00_01DType_00_01Arch_01_4.html#ad8fa7277ea33a870ba3285334dd204c0">mshadow::packet::PacketOp&lt; op::identity, DType, Arch &gt;::Map</a></div><div class="ttdeci">static MSHADOW_CINLINE Packet&lt; DType, Arch &gt; Map(const Packet&lt; DType, Arch &gt; &amp;src)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:199</div></div>
<div class="ttc" id="tensor_8h_html"><div class="ttname"><a href="tensor_8h.html">tensor.h</a></div><div class="ttdoc">header file of tensor data structure and functions This lib requires explicit memory allocation and d...</div></div>
<div class="ttc" id="structmshadow_1_1cpu_html"><div class="ttname"><a href="structmshadow_1_1cpu.html">mshadow::cpu</a></div><div class="ttdoc">device name CPU </div><div class="ttdef"><b>Definition:</b> tensor.h:39</div></div>
<div class="ttc" id="namespacemshadow_1_1expr_html_a0b4a783ea715eba66efea27dc443d9dc"><div class="ttname"><a href="namespacemshadow_1_1expr.html#a0b4a783ea715eba66efea27dc443d9dc">mshadow::expr::mask</a></div><div class="ttdeci">MaskExp&lt; IndexExp, SrcExp, DType &gt; mask(const Exp&lt; IndexExp, DType, e1 &gt; &amp;index, const Exp&lt; SrcExp, DType, e2 &gt; &amp;src)</div><div class="ttdef"><b>Definition:</b> mask.h:57</div></div>
<div class="ttc" id="expression_8h_html"><div class="ttname"><a href="expression_8h.html">expression.h</a></div><div class="ttdoc">definitions of abstract expressions and expressions template </div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4_html_afb3811e5983a4336f27fcef5673aba55"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#afb3811e5983a4336f27fcef5673aba55">mshadow::expr::PacketPlan&lt; Tensor&lt; Device, dim, DType &gt;, DType, Arch &gt;::Eval</a></div><div class="ttdeci">MSHADOW_CINLINE DType Eval(index_t y, index_t x) const</div><div class="ttdef"><b>Definition:</b> packet-inl.h:253</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1minus_00_01DType_00_01Arch_01_4_html_acd57bd12afecaa17569fc7e49f47e529"><div class="ttname"><a href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1minus_00_01DType_00_01Arch_01_4.html#acd57bd12afecaa17569fc7e49f47e529">mshadow::packet::PacketOp&lt; op::minus, DType, Arch &gt;::Map</a></div><div class="ttdeci">static MSHADOW_CINLINE Packet&lt; DType, Arch &gt; Map(const Packet&lt; DType, Arch &gt; &amp;lhs, const Packet&lt; DType, Arch &gt; &amp;rhs)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:174</div></div>
<div class="ttc" id="namespacemshadow_html_adcbc2e1131386fccb1474b0bdf045926"><div class="ttname"><a href="namespacemshadow.html#adcbc2e1131386fccb1474b0bdf045926">mshadow::index_t</a></div><div class="ttdeci">int32_t index_t</div><div class="ttdoc">type that will be used for index </div><div class="ttdef"><b>Definition:</b> base.h:343</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4_html_ab250f3402dc64b95bcf006f828e2876d"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#ab250f3402dc64b95bcf006f828e2876d">mshadow::expr::PacketPlan&lt; UnaryMapExp&lt; OP, TA, DType, etype &gt;, DType, Arch &gt;::PacketPlan</a></div><div class="ttdeci">PacketPlan(const PacketPlan&lt; TA, DType, Arch &gt; &amp;src)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:297</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4_html_a9cfa748d9f3eb611d178350a72724439"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a9cfa748d9f3eb611d178350a72724439">mshadow::expr::PacketPlan&lt; ScalarExp&lt; DType &gt;, DType, Arch &gt;::Eval</a></div><div class="ttdeci">MSHADOW_CINLINE DType Eval(index_t y, index_t x) const</div><div class="ttdef"><b>Definition:</b> packet-inl.h:269</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1mul_00_01DType_00_01Arch_01_4_html_abe5dd5265fb32b4982d4457987ba31c1"><div class="ttname"><a href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1mul_00_01DType_00_01Arch_01_4.html#abe5dd5265fb32b4982d4457987ba31c1">mshadow::packet::PacketOp&lt; op::mul, DType, Arch &gt;::Map</a></div><div class="ttdeci">static MSHADOW_CINLINE Packet&lt; DType, Arch &gt; Map(const Packet&lt; DType, Arch &gt; &amp;lhs, const Packet&lt; DType, Arch &gt; &amp;rhs)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:182</div></div>
<div class="ttc" id="structmshadow_1_1Tensor_html_a48a5927e810fbc45e43e92cfe397d9f2"><div class="ttname"><a href="structmshadow_1_1Tensor.html#a48a5927e810fbc45e43e92cfe397d9f2">mshadow::Tensor::FlatTo2D</a></div><div class="ttdeci">MSHADOW_XINLINE Tensor&lt; Device, 2, DType &gt; FlatTo2D(void) const</div><div class="ttdoc">flatten the tensor to 2 dimension, collapse the higher dimensions together </div><div class="ttdef"><b>Definition:</b> tensor.h:519</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01710a64b86afbf8d7faec025f10b905b0_html_acbddc0995f0dea05454823f29fac922b"><div class="ttname"><a href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01710a64b86afbf8d7faec025f10b905b0.html#acbddc0995f0dea05454823f29fac922b">mshadow::expr::PacketAlignCheck&lt; dim, BinaryMapExp&lt; OP, TA, TB, DType, etype &gt;, Arch &gt;::Check</a></div><div class="ttdeci">static bool Check(const BinaryMapExp&lt; OP, TA, TB, DType, etype &gt; &amp;t)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:406</div></div>
<div class="ttc" id="namespacemshadow_1_1packet_html_a69941771d29a1ae9a744c3e6c8b4ab4fa80fe267c1a066b1e78b8fce65a9db19e"><div class="ttname"><a href="namespacemshadow_1_1packet.html#a69941771d29a1ae9a744c3e6c8b4ab4fa80fe267c1a066b1e78b8fce65a9db19e">mshadow::packet::kSSE2</a></div><div class="ttdef"><b>Definition:</b> packet-inl.h:43</div></div>
<div class="ttc" id="structmshadow_1_1Tensor_html_a88cbcae11653307bfa4c99804320b638"><div class="ttname"><a href="structmshadow_1_1Tensor.html#a88cbcae11653307bfa4c99804320b638">mshadow::Tensor::size</a></div><div class="ttdeci">MSHADOW_XINLINE index_t size(int idx) const</div><div class="ttdoc">return size of i-th dimension, start counting from highest dimension </div><div class="ttdef"><b>Definition:</b> tensor.h:505</div></div>
<div class="ttc" id="sse-inl_8h_html"><div class="ttname"><a href="sse-inl_8h.html">sse-inl.h</a></div><div class="ttdoc">support of sse2 packet optimization of some operations </div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1Saver_3_01sv_1_1saveto_00_01TFloat_00_01Arch_01_4_html_a84e7afff8d944df0d90a35a5057f411a"><div class="ttname"><a href="structmshadow_1_1packet_1_1Saver_3_01sv_1_1saveto_00_01TFloat_00_01Arch_01_4.html#a84e7afff8d944df0d90a35a5057f411a">mshadow::packet::Saver&lt; sv::saveto, TFloat, Arch &gt;::Save</a></div><div class="ttdeci">static MSHADOW_CINLINE void Save(TFloat *dst, const Packet&lt; TFloat, Arch &gt; &amp;src)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:216</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1PacketOp_html"><div class="ttname"><a href="structmshadow_1_1packet_1_1PacketOp.html">mshadow::packet::PacketOp</a></div><div class="ttdoc">generic Packet operator </div><div class="ttdef"><b>Definition:</b> packet-inl.h:159</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4_html_a09971871cc9eb76783f035d74e1dbd2e"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a09971871cc9eb76783f035d74e1dbd2e">mshadow::expr::PacketPlan&lt; UnaryMapExp&lt; OP, TA, DType, etype &gt;, DType, Arch &gt;::EvalPacket</a></div><div class="ttdeci">MSHADOW_CINLINE packet::Packet&lt; DType &gt; EvalPacket(index_t y, index_t x) const</div><div class="ttdef"><b>Definition:</b> packet-inl.h:298</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4_html_a5dc48ea66a3dafff0751e2133bc8b775"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a5dc48ea66a3dafff0751e2133bc8b775">mshadow::expr::PacketPlan&lt; ScalarExp&lt; DType &gt;, DType, Arch &gt;::PacketPlan</a></div><div class="ttdeci">PacketPlan(DType scalar)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:265</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4_html_a9a03e9d164513ab1f1ec84465a7a7ca4"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01ScalarExp_3_01DType_01_4_00_01DType_00_01Arch_01_4.html#a9a03e9d164513ab1f1ec84465a7a7ca4">mshadow::expr::PacketPlan&lt; ScalarExp&lt; DType &gt;, DType, Arch &gt;::EvalPacket</a></div><div class="ttdeci">MSHADOW_CINLINE packet::Packet&lt; DType, Arch &gt; EvalPacket(index_t y, index_t x) const</div><div class="ttdef"><b>Definition:</b> packet-inl.h:266</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4_html_ae7b06a333d377c584ed000b426b105cd"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#ae7b06a333d377c584ed000b426b105cd">mshadow::expr::PacketPlan&lt; Tensor&lt; Device, dim, DType &gt;, DType, Arch &gt;::PacketPlan</a></div><div class="ttdeci">PacketPlan(const Tensor&lt; Device, dim, DType &gt; &amp;t)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:248</div></div>
<div class="ttc" id="namespacemshadow_1_1packet_html_a60f184b1173bb7f18db29856ba1b5107"><div class="ttname"><a href="namespacemshadow_1_1packet.html#a60f184b1173bb7f18db29856ba1b5107">mshadow::packet::CheckAlign</a></div><div class="ttdeci">bool CheckAlign(size_t pitch)</div><div class="ttdoc">check if a pointer is aligned </div><div class="ttdef"><b>Definition:</b> packet-inl.h:116</div></div>
<div class="ttc" id="namespacemshadow_1_1packet_html_aae366b300131f5212f480e9602ea232e"><div class="ttname"><a href="namespacemshadow_1_1packet.html#aae366b300131f5212f480e9602ea232e">mshadow::packet::LowerAlign</a></div><div class="ttdeci">index_t LowerAlign(index_t size)</div><div class="ttdoc">get lower bound of aligned index of size </div><div class="ttdef"><b>Definition:</b> packet-inl.h:146</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1AlignBytes_html"><div class="ttname"><a href="structmshadow_1_1packet_1_1AlignBytes.html">mshadow::packet::AlignBytes</a></div><div class="ttdef"><b>Definition:</b> packet-inl.h:62</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1UnaryMapExp_html_a2916051247ff9e5f1ff4c5020738d36c"><div class="ttname"><a href="structmshadow_1_1expr_1_1UnaryMapExp.html#a2916051247ff9e5f1ff4c5020738d36c">mshadow::expr::UnaryMapExp::src_</a></div><div class="ttdeci">const TA &amp; src_</div><div class="ttdoc">source expression </div><div class="ttdef"><b>Definition:</b> expression.h:407</div></div>
<div class="ttc" id="3rdparty_2mshadow_2mshadow_2base_8h_html_ae3f37fc5e892a11db794e475fae404a8"><div class="ttname"><a href="3rdparty_2mshadow_2mshadow_2base_8h.html#ae3f37fc5e892a11db794e475fae404a8">MSHADOW_CINLINE</a></div><div class="ttdeci">#define MSHADOW_CINLINE</div><div class="ttdoc">cpu force inline </div><div class="ttdef"><b>Definition:</b> base.h:233</div></div>
<div class="ttc" id="namespacemshadow_1_1packet_html_a3673b9721702cf91bb412810357417a7"><div class="ttname"><a href="namespacemshadow_1_1packet.html#a3673b9721702cf91bb412810357417a7">mshadow::packet::UpperAlign</a></div><div class="ttdeci">index_t UpperAlign(index_t size)</div><div class="ttdoc">get upper bound of aligned index of size </div><div class="ttdef"><b>Definition:</b> packet-inl.h:133</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1UnaryMapExp_html"><div class="ttname"><a href="structmshadow_1_1expr_1_1UnaryMapExp.html">mshadow::expr::UnaryMapExp</a></div><div class="ttdoc">unary map expression op(src) </div><div class="ttdef"><b>Definition:</b> expression.h:404</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1ScalarExp_html"><div class="ttname"><a href="structmshadow_1_1expr_1_1ScalarExp.html">mshadow::expr::ScalarExp</a></div><div class="ttdoc">scalar expression </div><div class="ttdef"><b>Definition:</b> expression.h:95</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1Saver_html"><div class="ttname"><a href="structmshadow_1_1packet_1_1Saver.html">mshadow::packet::Saver</a></div><div class="ttdef"><b>Definition:</b> packet-inl.h:207</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1MakeTensorExp_html_adf83aad5be17b50320bfcc6430244439"><div class="ttname"><a href="structmshadow_1_1expr_1_1MakeTensorExp.html#adf83aad5be17b50320bfcc6430244439">mshadow::expr::MakeTensorExp::real_self</a></div><div class="ttdeci">const SubType &amp; real_self(void) const</div><div class="ttdoc">true self of subtype </div><div class="ttdef"><b>Definition:</b> expr_engine-inl.h:49</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1Saver_html_a7dec82ec976e778f52332accf5332109"><div class="ttname"><a href="structmshadow_1_1packet_1_1Saver.html#a7dec82ec976e778f52332accf5332109">mshadow::packet::Saver::Save</a></div><div class="ttdeci">static MSHADOW_CINLINE void Save(TFloat *dst, const Packet&lt; TFloat, Arch &gt; &amp;src)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:208</div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1plus_00_01DType_00_01Arch_01_4_html_a0bec3da978e42d7e14e3c0dd10265bfe"><div class="ttname"><a href="structmshadow_1_1packet_1_1PacketOp_3_01op_1_1plus_00_01DType_00_01Arch_01_4.html#a0bec3da978e42d7e14e3c0dd10265bfe">mshadow::packet::PacketOp&lt; op::plus, DType, Arch &gt;::Map</a></div><div class="ttdeci">static MSHADOW_CINLINE Packet&lt; DType, Arch &gt; Map(const Packet&lt; DType, Arch &gt; &amp;lhs, const Packet&lt; DType, Arch &gt; &amp;rhs)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:166</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4_html_a15cff8316690eef649844d647df4bc60"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01BinaryMapExp_3_01OP_00_01TA_00_01TB_00_01DType_00_01etype_01_4_00_01DType_00_01Arch_01_4.html#a15cff8316690eef649844d647df4bc60">mshadow::expr::PacketPlan&lt; BinaryMapExp&lt; OP, TA, TB, DType, etype &gt;, DType, Arch &gt;::EvalPacket</a></div><div class="ttdeci">MSHADOW_CINLINE packet::Packet&lt; DType, Arch &gt; EvalPacket(index_t y, index_t x) const</div><div class="ttdef"><b>Definition:</b> packet-inl.h:282</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1MakeTensorExp_html"><div class="ttname"><a href="structmshadow_1_1expr_1_1MakeTensorExp.html">mshadow::expr::MakeTensorExp</a></div><div class="ttdoc">a general class that allows extension that makes tensors of some shape </div><div class="ttdef"><b>Definition:</b> expr_engine-inl.h:43</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1BinaryMapExp_html_ae4d3d912e56bbad508abeeed4743c38c"><div class="ttname"><a href="structmshadow_1_1expr_1_1BinaryMapExp.html#ae4d3d912e56bbad508abeeed4743c38c">mshadow::expr::BinaryMapExp::lhs_</a></div><div class="ttdeci">const TA &amp; lhs_</div><div class="ttdoc">left operand </div><div class="ttdef"><b>Definition:</b> expression.h:337</div></div>
<div class="ttc" id="namespacemshadow_html"><div class="ttname"><a href="namespacemshadow.html">mshadow</a></div><div class="ttdoc">overloaded + operator between half_t and bf16_t </div><div class="ttdef"><b>Definition:</b> base.h:334</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_html_a9f13cc90187ac190d0e336c6b9cd20a3"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan.html#a9f13cc90187ac190d0e336c6b9cd20a3">mshadow::expr::PacketPlan::EvalPacket</a></div><div class="ttdeci">MSHADOW_CINLINE packet::Packet&lt; DType, Arch &gt; EvalPacket(index_t y, index_t x) const</div><div class="ttdoc">evaluate the expression at index [y][x], x will be aligned to Packet&lt;DType, Arch&gt;::Size() ...</div></div>
<div class="ttc" id="structmshadow_1_1Tensor_html_afee556f188e29bbd0ecc45fe98d3c1c3"><div class="ttname"><a href="structmshadow_1_1Tensor.html#afee556f188e29bbd0ecc45fe98d3c1c3">mshadow::Tensor::stride_</a></div><div class="ttdeci">index_t stride_</div><div class="ttdoc">storing the stride information in x dimension this is used to deal with pitch allocation in gpu or ss...</div><div class="ttdef"><b>Definition:</b> tensor.h:441</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01Arch_01_4_html_ae4fd9e0d56b69e959ace381a8c11f329"><div class="ttname"><a href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01UnaryMapExp_3_01OP_00_01TA_00_01DType_00_01etype_01_4_00_01Arch_01_4.html#ae4fd9e0d56b69e959ace381a8c11f329">mshadow::expr::PacketAlignCheck&lt; dim, UnaryMapExp&lt; OP, TA, DType, etype &gt;, Arch &gt;::Check</a></div><div class="ttdeci">static bool Check(const UnaryMapExp&lt; OP, TA, DType, etype &gt; &amp;t)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:399</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4_html_a1252b3fd619aa1e7533077c150d8c4c3"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan_3_01Tensor_3_01Device_00_01dim_00_01DType_01_4_00_01DType_00_01Arch_01_4.html#a1252b3fd619aa1e7533077c150d8c4c3">mshadow::expr::PacketPlan&lt; Tensor&lt; Device, dim, DType &gt;, DType, Arch &gt;::EvalPacket</a></div><div class="ttdeci">MSHADOW_CINLINE packet::Packet&lt; DType, Arch &gt; EvalPacket(index_t y, index_t x) const</div><div class="ttdef"><b>Definition:</b> packet-inl.h:250</div></div>
<div class="ttc" id="structmshadow_1_1Tensor_html"><div class="ttname"><a href="structmshadow_1_1Tensor.html">mshadow::Tensor</a></div><div class="ttdoc">general tensor </div><div class="ttdef"><b>Definition:</b> tensor.h:420</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01Tensor_3_01cpu_00_01dim_00_01DType_01_4_00_01Arch_01_4_html_af613d87cfd68b9bd4f01895dadf38014"><div class="ttname"><a href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01Tensor_3_01cpu_00_01dim_00_01DType_01_4_00_01Arch_01_4.html#af613d87cfd68b9bd4f01895dadf38014">mshadow::expr::PacketAlignCheck&lt; dim, Tensor&lt; cpu, dim, DType &gt;, Arch &gt;::Check</a></div><div class="ttdeci">static bool Check(const Tensor&lt; cpu, dim, DType &gt; &amp;t)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:392</div></div>
<div class="ttc" id="3rdparty_2mshadow_2mshadow_2base_8h_html"><div class="ttname"><a href="3rdparty_2mshadow_2mshadow_2base_8h.html">base.h</a></div></div>
<div class="ttc" id="namespacemshadow_1_1expr_html_a8fb88661f1972b4614493ba09934fc1b"><div class="ttname"><a href="namespacemshadow_1_1expr.html#a8fb88661f1972b4614493ba09934fc1b">mshadow::expr::MapPacketPlan</a></div><div class="ttdeci">void MapPacketPlan(Tensor&lt; cpu, dim, DType &gt; _dst, const expr::PacketPlan&lt; E, DType, Arch &gt; &amp;plan)</div><div class="ttdoc">use PacketPlan to compute result </div><div class="ttdef"><b>Definition:</b> packet-inl.h:416</div></div>
<div class="ttc" id="plain-inl_8h_html"><div class="ttname"><a href="plain-inl_8h.html">plain-inl.h</a></div><div class="ttdoc">support of plain packet that use the plain datatype. </div></div>
<div class="ttc" id="structmshadow_1_1packet_1_1Packet_html"><div class="ttname"><a href="structmshadow_1_1packet_1_1Packet.html">mshadow::packet::Packet</a></div><div class="ttdoc">Generic packet type. </div><div class="ttdef"><b>Definition:</b> packet-inl.h:59</div></div>
<div class="ttc" id="classmshadow_1_1expr_1_1PacketPlan_html_a020eee5397c1126cd1ae354bb8b59149"><div class="ttname"><a href="classmshadow_1_1expr_1_1PacketPlan.html#a020eee5397c1126cd1ae354bb8b59149">mshadow::expr::PacketPlan::Eval</a></div><div class="ttdeci">MSHADOW_CINLINE DType Eval(index_t y, index_t x) const</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01ScalarExp_3_01DType_01_4_00_01Arch_01_4_html_a408f18d184aebd10227649a1d40a3e86"><div class="ttname"><a href="structmshadow_1_1expr_1_1PacketAlignCheck_3_01dim_00_01ScalarExp_3_01DType_01_4_00_01Arch_01_4.html#a408f18d184aebd10227649a1d40a3e86">mshadow::expr::PacketAlignCheck&lt; dim, ScalarExp&lt; DType &gt;, Arch &gt;::Check</a></div><div class="ttdeci">static bool Check(const ScalarExp&lt; DType &gt; &amp;exp)</div><div class="ttdef"><b>Definition:</b> packet-inl.h:386</div></div>
<div class="ttc" id="namespacemshadow_html_aa94c153a2f8bcd10be82a4f5598ae5b9"><div class="ttname"><a href="namespacemshadow.html#aa94c153a2f8bcd10be82a4f5598ae5b9">mshadow::openmp_index_t</a></div><div class="ttdeci">index_t openmp_index_t</div><div class="ttdoc">openmp index for linux </div><div class="ttdef"><b>Definition:</b> base.h:351</div></div>
<div class="ttc" id="structmshadow_1_1expr_1_1PacketCheck_html"><div class="ttname"><a href="structmshadow_1_1expr_1_1PacketCheck.html">mshadow::expr::PacketCheck</a></div><div class="ttdoc">static check packet enable </div><div class="ttdef"><b>Definition:</b> packet-inl.h:346</div></div>
</div><!-- fragment --></div><!-- contents -->
<!-- start footer part -->
<hr class="footer"/><address class="footer"><small>
Generated on Thu Jan 5 2023 00:58:42 for mxnet by &#160;<a href="http://www.doxygen.org/index.html">
<img class="footer" src="doxygen.png" alt="doxygen"/>
</a> 1.8.13
</small></address>
</body>
</html>