This contains my bachelors thesis and associated tex files, code snippets and maybe more. Topic: Data Movement in Heterogeneous Memories with Intel Data Streaming Accelerator
You can not select more than 25 topics Topics must start with a letter or number, can include dashes ('-') and can be up to 35 characters long.

2385 lines
111 KiB

  1. <?xml version="1.0" standalone="no"?>
  2. <!DOCTYPE svg PUBLIC "-//W3C//DTD SVG 1.1//EN" "http://www.w3.org/Graphics/SVG/1.1/DTD/svg11.dtd">
  3. <svg version="1.1" width="1200" height="646" onload="init(evt)" viewBox="0 0 1200 646" xmlns="http://www.w3.org/2000/svg" xmlns:xlink="http://www.w3.org/1999/xlink">
  4. <!-- Flame graph stack visualization. See https://github.com/brendangregg/FlameGraph for latest version, and http://www.brendangregg.com/flamegraphs.html for examples. -->
  5. <!-- NOTES: -->
  6. <defs>
  7. <linearGradient id="background" y1="0" y2="1" x1="0" x2="0" >
  8. <stop stop-color="#eeeeee" offset="5%" />
  9. <stop stop-color="#eeeeb0" offset="95%" />
  10. </linearGradient>
  11. </defs>
  12. <style type="text/css">
  13. text { font-family:Verdana; font-size:12px; fill:rgb(0,0,0); }
  14. #search, #ignorecase { opacity:0.1; cursor:pointer; }
  15. #search:hover, #search.show, #ignorecase:hover, #ignorecase.show { opacity:1; }
  16. #subtitle { text-anchor:middle; font-color:rgb(160,160,160); }
  17. #title { text-anchor:middle; font-size:17px}
  18. #unzoom { cursor:pointer; }
  19. #frames > *:hover { stroke:black; stroke-width:0.5; cursor:pointer; }
  20. .hide { display:none; }
  21. .parent { opacity:0.5; }
  22. </style>
  23. <script type="text/ecmascript">
  24. <![CDATA[
  25. "use strict";
  26. var details, searchbtn, unzoombtn, matchedtxt, svg, searching, currentSearchTerm, ignorecase, ignorecaseBtn;
  27. function init(evt) {
  28. details = document.getElementById("details").firstChild;
  29. searchbtn = document.getElementById("search");
  30. ignorecaseBtn = document.getElementById("ignorecase");
  31. unzoombtn = document.getElementById("unzoom");
  32. matchedtxt = document.getElementById("matched");
  33. svg = document.getElementsByTagName("svg")[0];
  34. searching = 0;
  35. currentSearchTerm = null;
  36. // use GET parameters to restore a flamegraphs state.
  37. var params = get_params();
  38. if (params.x && params.y)
  39. zoom(find_group(document.querySelector('[x="' + params.x + '"][y="' + params.y + '"]')));
  40. if (params.s) search(params.s);
  41. }
  42. // event listeners
  43. window.addEventListener("click", function(e) {
  44. var target = find_group(e.target);
  45. if (target) {
  46. if (target.nodeName == "a") {
  47. if (e.ctrlKey === false) return;
  48. e.preventDefault();
  49. }
  50. if (target.classList.contains("parent")) unzoom(true);
  51. zoom(target);
  52. if (!document.querySelector('.parent')) {
  53. // we have basically done a clearzoom so clear the url
  54. var params = get_params();
  55. if (params.x) delete params.x;
  56. if (params.y) delete params.y;
  57. history.replaceState(null, null, parse_params(params));
  58. unzoombtn.classList.add("hide");
  59. return;
  60. }
  61. // set parameters for zoom state
  62. var el = target.querySelector("rect");
  63. if (el && el.attributes && el.attributes.y && el.attributes._orig_x) {
  64. var params = get_params()
  65. params.x = el.attributes._orig_x.value;
  66. params.y = el.attributes.y.value;
  67. history.replaceState(null, null, parse_params(params));
  68. }
  69. }
  70. else if (e.target.id == "unzoom") clearzoom();
  71. else if (e.target.id == "search") search_prompt();
  72. else if (e.target.id == "ignorecase") toggle_ignorecase();
  73. }, false)
  74. // mouse-over for info
  75. // show
  76. window.addEventListener("mouseover", function(e) {
  77. var target = find_group(e.target);
  78. if (target) details.nodeValue = "Function: " + g_to_text(target);
  79. }, false)
  80. // clear
  81. window.addEventListener("mouseout", function(e) {
  82. var target = find_group(e.target);
  83. if (target) details.nodeValue = ' ';
  84. }, false)
  85. // ctrl-F for search
  86. // ctrl-I to toggle case-sensitive search
  87. window.addEventListener("keydown",function (e) {
  88. if (e.keyCode === 114 || (e.ctrlKey && e.keyCode === 70)) {
  89. e.preventDefault();
  90. search_prompt();
  91. }
  92. else if (e.ctrlKey && e.keyCode === 73) {
  93. e.preventDefault();
  94. toggle_ignorecase();
  95. }
  96. }, false)
  97. // functions
  98. function get_params() {
  99. var params = {};
  100. var paramsarr = window.location.search.substr(1).split('&');
  101. for (var i = 0; i < paramsarr.length; ++i) {
  102. var tmp = paramsarr[i].split("=");
  103. if (!tmp[0] || !tmp[1]) continue;
  104. params[tmp[0]] = decodeURIComponent(tmp[1]);
  105. }
  106. return params;
  107. }
  108. function parse_params(params) {
  109. var uri = "?";
  110. for (var key in params) {
  111. uri += key + '=' + encodeURIComponent(params[key]) + '&';
  112. }
  113. if (uri.slice(-1) == "&")
  114. uri = uri.substring(0, uri.length - 1);
  115. if (uri == '?')
  116. uri = window.location.href.split('?')[0];
  117. return uri;
  118. }
  119. function find_child(node, selector) {
  120. var children = node.querySelectorAll(selector);
  121. if (children.length) return children[0];
  122. }
  123. function find_group(node) {
  124. var parent = node.parentElement;
  125. if (!parent) return;
  126. if (parent.id == "frames") return node;
  127. return find_group(parent);
  128. }
  129. function orig_save(e, attr, val) {
  130. if (e.attributes["_orig_" + attr] != undefined) return;
  131. if (e.attributes[attr] == undefined) return;
  132. if (val == undefined) val = e.attributes[attr].value;
  133. e.setAttribute("_orig_" + attr, val);
  134. }
  135. function orig_load(e, attr) {
  136. if (e.attributes["_orig_"+attr] == undefined) return;
  137. e.attributes[attr].value = e.attributes["_orig_" + attr].value;
  138. e.removeAttribute("_orig_"+attr);
  139. }
  140. function g_to_text(e) {
  141. var text = find_child(e, "title").firstChild.nodeValue;
  142. return (text)
  143. }
  144. function g_to_func(e) {
  145. var func = g_to_text(e);
  146. // if there's any manipulation we want to do to the function
  147. // name before it's searched, do it here before returning.
  148. return (func);
  149. }
  150. function update_text(e) {
  151. var r = find_child(e, "rect");
  152. var t = find_child(e, "text");
  153. var w = parseFloat(r.attributes.width.value) -3;
  154. var txt = find_child(e, "title").textContent.replace(/\([^(]*\)$/,"");
  155. t.attributes.x.value = parseFloat(r.attributes.x.value) + 3;
  156. // Smaller than this size won't fit anything
  157. if (w < 2 * 12 * 0.59) {
  158. t.textContent = "";
  159. return;
  160. }
  161. t.textContent = txt;
  162. var sl = t.getSubStringLength(0, txt.length);
  163. // check if only whitespace or if we can fit the entire string into width w
  164. if (/^ *$/.test(txt) || sl < w)
  165. return;
  166. // this isn't perfect, but gives a good starting point
  167. // and avoids calling getSubStringLength too often
  168. var start = Math.floor((w/sl) * txt.length);
  169. for (var x = start; x > 0; x = x-2) {
  170. if (t.getSubStringLength(0, x + 2) <= w) {
  171. t.textContent = txt.substring(0, x) + "..";
  172. return;
  173. }
  174. }
  175. t.textContent = "";
  176. }
  177. // zoom
  178. function zoom_reset(e) {
  179. if (e.attributes != undefined) {
  180. orig_load(e, "x");
  181. orig_load(e, "width");
  182. }
  183. if (e.childNodes == undefined) return;
  184. for (var i = 0, c = e.childNodes; i < c.length; i++) {
  185. zoom_reset(c[i]);
  186. }
  187. }
  188. function zoom_child(e, x, ratio) {
  189. if (e.attributes != undefined) {
  190. if (e.attributes.x != undefined) {
  191. orig_save(e, "x");
  192. e.attributes.x.value = (parseFloat(e.attributes.x.value) - x - 10) * ratio + 10;
  193. if (e.tagName == "text")
  194. e.attributes.x.value = find_child(e.parentNode, "rect[x]").attributes.x.value + 3;
  195. }
  196. if (e.attributes.width != undefined) {
  197. orig_save(e, "width");
  198. e.attributes.width.value = parseFloat(e.attributes.width.value) * ratio;
  199. }
  200. }
  201. if (e.childNodes == undefined) return;
  202. for (var i = 0, c = e.childNodes; i < c.length; i++) {
  203. zoom_child(c[i], x - 10, ratio);
  204. }
  205. }
  206. function zoom_parent(e) {
  207. if (e.attributes) {
  208. if (e.attributes.x != undefined) {
  209. orig_save(e, "x");
  210. e.attributes.x.value = 10;
  211. }
  212. if (e.attributes.width != undefined) {
  213. orig_save(e, "width");
  214. e.attributes.width.value = parseInt(svg.width.baseVal.value) - (10 * 2);
  215. }
  216. }
  217. if (e.childNodes == undefined) return;
  218. for (var i = 0, c = e.childNodes; i < c.length; i++) {
  219. zoom_parent(c[i]);
  220. }
  221. }
  222. function zoom(node) {
  223. var attr = find_child(node, "rect").attributes;
  224. var width = parseFloat(attr.width.value);
  225. var xmin = parseFloat(attr.x.value);
  226. var xmax = parseFloat(xmin + width);
  227. var ymin = parseFloat(attr.y.value);
  228. var ratio = (svg.width.baseVal.value - 2 * 10) / width;
  229. // XXX: Workaround for JavaScript float issues (fix me)
  230. var fudge = 0.0001;
  231. unzoombtn.classList.remove("hide");
  232. var el = document.getElementById("frames").children;
  233. for (var i = 0; i < el.length; i++) {
  234. var e = el[i];
  235. var a = find_child(e, "rect").attributes;
  236. var ex = parseFloat(a.x.value);
  237. var ew = parseFloat(a.width.value);
  238. var upstack;
  239. // Is it an ancestor
  240. if (0 == 0) {
  241. upstack = parseFloat(a.y.value) > ymin;
  242. } else {
  243. upstack = parseFloat(a.y.value) < ymin;
  244. }
  245. if (upstack) {
  246. // Direct ancestor
  247. if (ex <= xmin && (ex+ew+fudge) >= xmax) {
  248. e.classList.add("parent");
  249. zoom_parent(e);
  250. update_text(e);
  251. }
  252. // not in current path
  253. else
  254. e.classList.add("hide");
  255. }
  256. // Children maybe
  257. else {
  258. // no common path
  259. if (ex < xmin || ex + fudge >= xmax) {
  260. e.classList.add("hide");
  261. }
  262. else {
  263. zoom_child(e, xmin, ratio);
  264. update_text(e);
  265. }
  266. }
  267. }
  268. search();
  269. }
  270. function unzoom(dont_update_text) {
  271. unzoombtn.classList.add("hide");
  272. var el = document.getElementById("frames").children;
  273. for(var i = 0; i < el.length; i++) {
  274. el[i].classList.remove("parent");
  275. el[i].classList.remove("hide");
  276. zoom_reset(el[i]);
  277. if(!dont_update_text) update_text(el[i]);
  278. }
  279. search();
  280. }
  281. function clearzoom() {
  282. unzoom();
  283. // remove zoom state
  284. var params = get_params();
  285. if (params.x) delete params.x;
  286. if (params.y) delete params.y;
  287. history.replaceState(null, null, parse_params(params));
  288. }
  289. // search
  290. function toggle_ignorecase() {
  291. ignorecase = !ignorecase;
  292. if (ignorecase) {
  293. ignorecaseBtn.classList.add("show");
  294. } else {
  295. ignorecaseBtn.classList.remove("show");
  296. }
  297. reset_search();
  298. search();
  299. }
  300. function reset_search() {
  301. var el = document.querySelectorAll("#frames rect");
  302. for (var i = 0; i < el.length; i++) {
  303. orig_load(el[i], "fill")
  304. }
  305. var params = get_params();
  306. delete params.s;
  307. history.replaceState(null, null, parse_params(params));
  308. }
  309. function search_prompt() {
  310. if (!searching) {
  311. var term = prompt("Enter a search term (regexp " +
  312. "allowed, eg: ^ext4_)"
  313. + (ignorecase ? ", ignoring case" : "")
  314. + "\nPress Ctrl-i to toggle case sensitivity", "");
  315. if (term != null) search(term);
  316. } else {
  317. reset_search();
  318. searching = 0;
  319. currentSearchTerm = null;
  320. searchbtn.classList.remove("show");
  321. searchbtn.firstChild.nodeValue = "Search"
  322. matchedtxt.classList.add("hide");
  323. matchedtxt.firstChild.nodeValue = ""
  324. }
  325. }
  326. function search(term) {
  327. if (term) currentSearchTerm = term;
  328. var re = new RegExp(currentSearchTerm, ignorecase ? 'i' : '');
  329. var el = document.getElementById("frames").children;
  330. var matches = new Object();
  331. var maxwidth = 0;
  332. for (var i = 0; i < el.length; i++) {
  333. var e = el[i];
  334. var func = g_to_func(e);
  335. var rect = find_child(e, "rect");
  336. if (func == null || rect == null)
  337. continue;
  338. // Save max width. Only works as we have a root frame
  339. var w = parseFloat(rect.attributes.width.value);
  340. if (w > maxwidth)
  341. maxwidth = w;
  342. if (func.match(re)) {
  343. // highlight
  344. var x = parseFloat(rect.attributes.x.value);
  345. orig_save(rect, "fill");
  346. rect.attributes.fill.value = "rgb(230,0,230)";
  347. // remember matches
  348. if (matches[x] == undefined) {
  349. matches[x] = w;
  350. } else {
  351. if (w > matches[x]) {
  352. // overwrite with parent
  353. matches[x] = w;
  354. }
  355. }
  356. searching = 1;
  357. }
  358. }
  359. if (!searching)
  360. return;
  361. var params = get_params();
  362. params.s = currentSearchTerm;
  363. history.replaceState(null, null, parse_params(params));
  364. searchbtn.classList.add("show");
  365. searchbtn.firstChild.nodeValue = "Reset Search";
  366. // calculate percent matched, excluding vertical overlap
  367. var count = 0;
  368. var lastx = -1;
  369. var lastw = 0;
  370. var keys = Array();
  371. for (k in matches) {
  372. if (matches.hasOwnProperty(k))
  373. keys.push(k);
  374. }
  375. // sort the matched frames by their x location
  376. // ascending, then width descending
  377. keys.sort(function(a, b){
  378. return a - b;
  379. });
  380. // Step through frames saving only the biggest bottom-up frames
  381. // thanks to the sort order. This relies on the tree property
  382. // where children are always smaller than their parents.
  383. var fudge = 0.0001; // JavaScript floating point
  384. for (var k in keys) {
  385. var x = parseFloat(keys[k]);
  386. var w = matches[keys[k]];
  387. if (x >= lastx + lastw - fudge) {
  388. count += w;
  389. lastx = x;
  390. lastw = w;
  391. }
  392. }
  393. // display matched percent
  394. matchedtxt.classList.remove("hide");
  395. var pct = 100 * count / maxwidth;
  396. if (pct != 100) pct = pct.toFixed(1)
  397. matchedtxt.firstChild.nodeValue = "Matched: " + pct + "%";
  398. }
  399. ]]>
  400. </script>
  401. <rect x="0.0" y="0" width="1200.0" height="646.0" fill="url(#background)" />
  402. <text id="title" x="600.00" y="24" >Flame Graph</text>
  403. <text id="details" x="10.00" y="629" > </text>
  404. <text id="unzoom" x="10.00" y="24" class="hide">Reset Zoom</text>
  405. <text id="search" x="1090.00" y="24" >Search</text>
  406. <text id="ignorecase" x="1174.00" y="24" >ic</text>
  407. <text id="matched" x="1090.00" y="629" > </text>
  408. <g id="frames">
  409. <g >
  410. <title>release_pages (52,708,279 samples, 0.10%)</title><rect x="567.8" y="357" width="1.2" height="15.0" fill="rgb(228,106,25)" rx="2" ry="2" />
  411. <text x="570.78" y="367.5" ></text>
  412. </g>
  413. <g >
  414. <title>aggr_j (6,104,856,818 samples, 11.92%)</title><rect x="867.1" y="517" width="140.7" height="15.0" fill="rgb(221,75,17)" rx="2" ry="2" />
  415. <text x="870.12" y="527.5" >aggr_j</text>
  416. </g>
  417. <g >
  418. <title>dml::core::dispatcher::hw_device::initialize_new_device (10,597,924 samples, 0.02%)</title><rect x="1133.3" y="325" width="0.3" height="15.0" fill="rgb(242,174,41)" rx="2" ry="2" />
  419. <text x="1136.31" y="335.5" ></text>
  420. </g>
  421. <g >
  422. <title>cgroup_rstat_updated (260,795,386 samples, 0.51%)</title><rect x="458.3" y="325" width="6.1" height="15.0" fill="rgb(244,180,43)" rx="2" ry="2" />
  423. <text x="461.34" y="335.5" ></text>
  424. </g>
  425. <g >
  426. <title>free_unref_page_prepare (11,193,897 samples, 0.02%)</title><rect x="15.6" y="309" width="0.3" height="15.0" fill="rgb(238,155,37)" rx="2" ry="2" />
  427. <text x="18.64" y="319.5" ></text>
  428. </g>
  429. <g >
  430. <title>error_entry (19,445,388 samples, 0.04%)</title><rect x="147.1" y="485" width="0.4" height="15.0" fill="rgb(240,163,39)" rx="2" ry="2" />
  431. <text x="150.07" y="495.5" ></text>
  432. </g>
  433. <g >
  434. <title>__x64_sys_openat (4,893,850 samples, 0.01%)</title><rect x="1133.3" y="149" width="0.1" height="15.0" fill="rgb(251,215,51)" rx="2" ry="2" />
  435. <text x="1136.32" y="159.5" ></text>
  436. </g>
  437. <g >
  438. <title>memcg_check_events (2,082,895,253 samples, 4.07%)</title><rect x="476.5" y="357" width="48.0" height="15.0" fill="rgb(206,4,1)" rx="2" ry="2" />
  439. <text x="479.54" y="367.5" >memc..</text>
  440. </g>
  441. <g >
  442. <title>__get_vma_policy (6,052,375 samples, 0.01%)</title><rect x="593.3" y="373" width="0.1" height="15.0" fill="rgb(210,27,6)" rx="2" ry="2" />
  443. <text x="596.27" y="383.5" ></text>
  444. </g>
  445. <g >
  446. <title>policy_node (11,237,982 samples, 0.02%)</title><rect x="593.4" y="373" width="0.3" height="15.0" fill="rgb(236,143,34)" rx="2" ry="2" />
  447. <text x="596.41" y="383.5" ></text>
  448. </g>
  449. <g >
  450. <title>__handle_mm_fault (1,740,573,708 samples, 3.40%)</title><rect x="92.5" y="421" width="40.1" height="15.0" fill="rgb(207,9,2)" rx="2" ry="2" />
  451. <text x="95.48" y="431.5" >__h..</text>
  452. </g>
  453. <g >
  454. <title>up_read (54,454,946 samples, 0.11%)</title><rect x="602.8" y="437" width="1.2" height="15.0" fill="rgb(209,18,4)" rx="2" ry="2" />
  455. <text x="605.77" y="447.5" ></text>
  456. </g>
  457. <g >
  458. <title>mmap_region (12,738,596 samples, 0.02%)</title><rect x="147.6" y="389" width="0.3" height="15.0" fill="rgb(231,121,28)" rx="2" ry="2" />
  459. <text x="150.59" y="399.5" ></text>
  460. </g>
  461. <g >
  462. <title>__mod_memcg_lruvec_state (18,251,466 samples, 0.04%)</title><rect x="119.8" y="357" width="0.5" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  463. <text x="122.84" y="367.5" ></text>
  464. </g>
  465. <g >
  466. <title>kthread_blkcg (5,187,501 samples, 0.01%)</title><rect x="422.5" y="357" width="0.1" height="15.0" fill="rgb(249,203,48)" rx="2" ry="2" />
  467. <text x="425.46" y="367.5" ></text>
  468. </g>
  469. <g >
  470. <title>__pte_alloc (4,825,833 samples, 0.01%)</title><rect x="109.5" y="389" width="0.1" height="15.0" fill="rgb(218,62,15)" rx="2" ry="2" />
  471. <text x="112.49" y="399.5" ></text>
  472. </g>
  473. <g >
  474. <title>__mem_cgroup_uncharge_list (24,144,483 samples, 0.05%)</title><rect x="31.3" y="309" width="0.5" height="15.0" fill="rgb(219,68,16)" rx="2" ry="2" />
  475. <text x="34.28" y="319.5" ></text>
  476. </g>
  477. <g >
  478. <title>folio_add_lru (612,805,660 samples, 1.20%)</title><rect x="555.2" y="389" width="14.1" height="15.0" fill="rgb(208,17,4)" rx="2" ry="2" />
  479. <text x="558.15" y="399.5" ></text>
  480. </g>
  481. <g >
  482. <title>_raw_spin_unlock (8,778,490 samples, 0.02%)</title><rect x="128.3" y="325" width="0.2" height="15.0" fill="rgb(223,85,20)" rx="2" ry="2" />
  483. <text x="131.33" y="335.5" ></text>
  484. </g>
  485. <g >
  486. <title>do_user_addr_fault (38,214,263 samples, 0.07%)</title><rect x="1126.6" y="453" width="0.9" height="15.0" fill="rgb(228,108,25)" rx="2" ry="2" />
  487. <text x="1129.59" y="463.5" ></text>
  488. </g>
  489. <g >
  490. <title>sysvec_apic_timer_interrupt (7,679,459 samples, 0.02%)</title><rect x="320.8" y="469" width="0.2" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  491. <text x="323.83" y="479.5" ></text>
  492. </g>
  493. <g >
  494. <title>__rcu_read_lock (24,197,159 samples, 0.05%)</title><rect x="552.5" y="357" width="0.6" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  495. <text x="555.52" y="367.5" ></text>
  496. </g>
  497. <g >
  498. <title>check_preemption_disabled (6,898,806 samples, 0.01%)</title><rect x="18.0" y="277" width="0.1" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  499. <text x="20.99" y="287.5" ></text>
  500. </g>
  501. <g >
  502. <title>qi_submit_sync (42,245,564 samples, 0.08%)</title><rect x="19.5" y="309" width="0.9" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  503. <text x="22.46" y="319.5" ></text>
  504. </g>
  505. <g >
  506. <title>check_preemption_disabled (19,006,854 samples, 0.04%)</title><rect x="557.5" y="373" width="0.5" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  507. <text x="560.52" y="383.5" ></text>
  508. </g>
  509. <g >
  510. <title>check_preemption_disabled (156,498,969 samples, 0.31%)</title><rect x="103.0" y="341" width="3.6" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  511. <text x="105.97" y="351.5" ></text>
  512. </g>
  513. <g >
  514. <title>get_mem_cgroup_from_mm (115,813,924 samples, 0.23%)</title><rect x="550.7" y="373" width="2.6" height="15.0" fill="rgb(218,61,14)" rx="2" ry="2" />
  515. <text x="553.67" y="383.5" ></text>
  516. </g>
  517. <g >
  518. <title>__next_zones_zonelist (40,627,227 samples, 0.08%)</title><rect x="579.4" y="341" width="0.9" height="15.0" fill="rgb(223,86,20)" rx="2" ry="2" />
  519. <text x="582.41" y="351.5" ></text>
  520. </g>
  521. <g >
  522. <title>__alloc_pages (374,402,804 samples, 0.73%)</title><rect x="122.1" y="357" width="8.6" height="15.0" fill="rgb(233,129,30)" rx="2" ry="2" />
  523. <text x="125.10" y="367.5" ></text>
  524. </g>
  525. <g >
  526. <title>dsacache::Cache::GetCacheNode (6,787,704 samples, 0.01%)</title><rect x="1128.1" y="485" width="0.2" height="15.0" fill="rgb(243,175,41)" rx="2" ry="2" />
  527. <text x="1131.12" y="495.5" ></text>
  528. </g>
  529. <g >
  530. <title>dsacache::Cache::GetCacheNode (19,011,999 samples, 0.04%)</title><rect x="1007.3" y="485" width="0.4" height="15.0" fill="rgb(243,175,41)" rx="2" ry="2" />
  531. <text x="1010.25" y="495.5" ></text>
  532. </g>
  533. <g >
  534. <title>change_protection (201,181,727 samples, 0.39%)</title><rect x="1128.4" y="117" width="4.7" height="15.0" fill="rgb(209,22,5)" rx="2" ry="2" />
  535. <text x="1131.43" y="127.5" ></text>
  536. </g>
  537. <g >
  538. <title>check_preemption_disabled (11,365,460 samples, 0.02%)</title><rect x="116.6" y="309" width="0.2" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  539. <text x="119.55" y="319.5" ></text>
  540. </g>
  541. <g >
  542. <title>__this_cpu_preempt_check (6,897,820 samples, 0.01%)</title><rect x="41.6" y="277" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  543. <text x="44.60" y="287.5" ></text>
  544. </g>
  545. <g >
  546. <title>__folio_throttle_swaprate (38,895,583 samples, 0.08%)</title><rect x="421.7" y="389" width="0.9" height="15.0" fill="rgb(239,160,38)" rx="2" ry="2" />
  547. <text x="424.68" y="399.5" ></text>
  548. </g>
  549. <g >
  550. <title>__this_cpu_preempt_check (12,203,410 samples, 0.02%)</title><rect x="102.7" y="341" width="0.3" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  551. <text x="105.69" y="351.5" ></text>
  552. </g>
  553. <g >
  554. <title>perf_iterate_ctx (7,917,062 samples, 0.02%)</title><rect x="147.7" y="341" width="0.2" height="15.0" fill="rgb(205,4,0)" rx="2" ry="2" />
  555. <text x="150.68" y="351.5" ></text>
  556. </g>
  557. <g >
  558. <title>vm_normal_page (16,383,619 samples, 0.03%)</title><rect x="43.2" y="341" width="0.4" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  559. <text x="46.23" y="351.5" ></text>
  560. </g>
  561. <g >
  562. <title>__rcu_read_lock (5,184,268 samples, 0.01%)</title><rect x="428.2" y="357" width="0.1" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  563. <text x="431.19" y="367.5" ></text>
  564. </g>
  565. <g >
  566. <title>vma_alloc_folio (737,893,285 samples, 1.44%)</title><rect x="577.4" y="389" width="17.0" height="15.0" fill="rgb(245,187,44)" rx="2" ry="2" />
  567. <text x="580.42" y="399.5" ></text>
  568. </g>
  569. <g >
  570. <title>unsigned long std::uniform_int_distribution&lt;unsigned long&gt;::operator (5,186,627 samples, 0.01%)</title><rect x="1133.9" y="517" width="0.1" height="15.0" fill="rgb(252,216,51)" rx="2" ry="2" />
  571. <text x="1136.89" y="527.5" ></text>
  572. </g>
  573. <g >
  574. <title>check_preemption_disabled (12,072,500 samples, 0.02%)</title><rect x="41.1" y="261" width="0.2" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  575. <text x="44.06" y="271.5" ></text>
  576. </g>
  577. <g >
  578. <title>__hrtimer_run_queues (16,533,531 samples, 0.03%)</title><rect x="1127.7" y="421" width="0.4" height="15.0" fill="rgb(237,150,35)" rx="2" ry="2" />
  579. <text x="1130.68" y="431.5" ></text>
  580. </g>
  581. <g >
  582. <title>__list_del_entry_valid (6,896,516 samples, 0.01%)</title><rect x="32.2" y="293" width="0.2" height="15.0" fill="rgb(239,158,37)" rx="2" ry="2" />
  583. <text x="35.22" y="303.5" ></text>
  584. </g>
  585. <g >
  586. <title>__GI___mmap64 (14,975,543 samples, 0.03%)</title><rect x="147.6" y="485" width="0.3" height="15.0" fill="rgb(221,77,18)" rx="2" ry="2" />
  587. <text x="150.58" y="495.5" ></text>
  588. </g>
  589. <g >
  590. <title>__mod_lruvec_state (28,519,367 samples, 0.06%)</title><rect x="565.5" y="325" width="0.6" height="15.0" fill="rgb(226,100,24)" rx="2" ry="2" />
  591. <text x="568.49" y="335.5" ></text>
  592. </g>
  593. <g >
  594. <title>charge_memcg (5,532,425,220 samples, 10.81%)</title><rect x="423.2" y="373" width="127.5" height="15.0" fill="rgb(242,170,40)" rx="2" ry="2" />
  595. <text x="426.15" y="383.5" >charge_memcg</text>
  596. </g>
  597. <g >
  598. <title>syscall (10,248,023 samples, 0.02%)</title><rect x="1007.5" y="469" width="0.2" height="15.0" fill="rgb(234,136,32)" rx="2" ry="2" />
  599. <text x="1010.45" y="479.5" ></text>
  600. </g>
  601. <g >
  602. <title>Aggregation&lt;unsigned long, Sum, (6,079,728,229 samples, 11.88%)</title><rect x="867.1" y="501" width="140.2" height="15.0" fill="rgb(251,215,51)" rx="2" ry="2" />
  603. <text x="870.12" y="511.5" >Aggregation&lt;unsig..</text>
  604. </g>
  605. <g >
  606. <title>check_preemption_disabled (24,263,995 samples, 0.05%)</title><rect x="133.5" y="389" width="0.6" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  607. <text x="136.53" y="399.5" ></text>
  608. </g>
  609. <g >
  610. <title>asm_exc_page_fault (4,003,098,524 samples, 7.82%)</title><rect x="54.8" y="485" width="92.3" height="15.0" fill="rgb(225,93,22)" rx="2" ry="2" />
  611. <text x="57.81" y="495.5" >asm_exc_pag..</text>
  612. </g>
  613. <g >
  614. <title>__folio_throttle_swaprate (22,634,579 samples, 0.04%)</title><rect x="94.8" y="389" width="0.5" height="15.0" fill="rgb(239,160,38)" rx="2" ry="2" />
  615. <text x="97.79" y="399.5" ></text>
  616. </g>
  617. <g >
  618. <title>p4d_offset (12,965,965 samples, 0.03%)</title><rect x="594.4" y="405" width="0.3" height="15.0" fill="rgb(214,45,10)" rx="2" ry="2" />
  619. <text x="597.42" y="415.5" ></text>
  620. </g>
  621. <g >
  622. <title>grow_heap (209,389,327 samples, 0.41%)</title><rect x="1128.4" y="229" width="4.9" height="15.0" fill="rgb(237,151,36)" rx="2" ry="2" />
  623. <text x="1131.43" y="239.5" ></text>
  624. </g>
  625. <g >
  626. <title>blk_cgroup_congested (20,052,243 samples, 0.04%)</title><rect x="94.8" y="373" width="0.5" height="15.0" fill="rgb(250,211,50)" rx="2" ry="2" />
  627. <text x="97.85" y="383.5" ></text>
  628. </g>
  629. <g >
  630. <title>do_filp_open (4,455,340 samples, 0.01%)</title><rect x="1133.3" y="117" width="0.1" height="15.0" fill="rgb(211,28,6)" rx="2" ry="2" />
  631. <text x="1136.32" y="127.5" ></text>
  632. </g>
  633. <g >
  634. <title>numa_bitmask_alloc (4,453,868 samples, 0.01%)</title><rect x="1007.3" y="453" width="0.1" height="15.0" fill="rgb(234,137,32)" rx="2" ry="2" />
  635. <text x="1010.27" y="463.5" ></text>
  636. </g>
  637. <g >
  638. <title>lru_gen_del_folio.constprop.0 (257,002,243 samples, 0.50%)</title><rect x="37.3" y="309" width="5.9" height="15.0" fill="rgb(224,91,21)" rx="2" ry="2" />
  639. <text x="40.30" y="319.5" ></text>
  640. </g>
  641. <g >
  642. <title>free_unref_page_list (232,831,460 samples, 0.45%)</title><rect x="31.9" y="309" width="5.4" height="15.0" fill="rgb(221,77,18)" rx="2" ry="2" />
  643. <text x="34.94" y="319.5" ></text>
  644. </g>
  645. <g >
  646. <title>qi_flush_dev_iotlb_pasid (27,600,815 samples, 0.05%)</title><rect x="10.6" y="325" width="0.6" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  647. <text x="13.55" y="335.5" ></text>
  648. </g>
  649. <g >
  650. <title>__this_cpu_preempt_check (5,174,961 samples, 0.01%)</title><rect x="15.0" y="261" width="0.1" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  651. <text x="17.97" y="271.5" ></text>
  652. </g>
  653. <g >
  654. <title>__this_cpu_preempt_check (9,488,485 samples, 0.02%)</title><rect x="40.8" y="261" width="0.3" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  655. <text x="43.84" y="271.5" ></text>
  656. </g>
  657. <g >
  658. <title>mprotect_fixup (208,874,517 samples, 0.41%)</title><rect x="1128.4" y="133" width="4.8" height="15.0" fill="rgb(236,144,34)" rx="2" ry="2" />
  659. <text x="1131.43" y="143.5" ></text>
  660. </g>
  661. <g >
  662. <title>QDPBench (51,196,000,579 samples, 100.00%)</title><rect x="10.0" y="581" width="1180.0" height="15.0" fill="rgb(233,131,31)" rx="2" ry="2" />
  663. <text x="13.00" y="591.5" >QDPBench</text>
  664. </g>
  665. <g >
  666. <title>inc_mm_counter (85,556,117 samples, 0.17%)</title><rect x="574.7" y="389" width="2.0" height="15.0" fill="rgb(238,153,36)" rx="2" ry="2" />
  667. <text x="577.73" y="399.5" ></text>
  668. </g>
  669. <g >
  670. <title>check_preemption_disabled (347,960,254 samples, 0.68%)</title><rect x="464.4" y="325" width="8.0" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  671. <text x="467.36" y="335.5" ></text>
  672. </g>
  673. <g >
  674. <title>std::__new_allocator&lt;dml::detail::ml::utils::structure_from&lt;dml::detail::descriptor, dml::detail::completion_record&gt; &gt;::allocate (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="325" width="5.0" height="15.0" fill="rgb(248,201,48)" rx="2" ry="2" />
  675. <text x="1131.30" y="335.5" ></text>
  676. </g>
  677. <g >
  678. <title>dml::core::dispatcher::hw_dispatcher::initialize_hw (11,868,621 samples, 0.02%)</title><rect x="1133.3" y="341" width="0.3" height="15.0" fill="rgb(242,173,41)" rx="2" ry="2" />
  679. <text x="1136.28" y="351.5" ></text>
  680. </g>
  681. <g >
  682. <title>advise_stack_range (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="533" width="0.1" height="15.0" fill="rgb(236,145,34)" rx="2" ry="2" />
  683. <text x="1136.69" y="543.5" ></text>
  684. </g>
  685. <g >
  686. <title>check_preemption_disabled (6,193,135 samples, 0.01%)</title><rect x="120.1" y="341" width="0.1" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  687. <text x="123.08" y="351.5" ></text>
  688. </g>
  689. <g >
  690. <title>exc_page_fault (8,328,027,484 samples, 16.27%)</title><rect x="412.2" y="469" width="192.0" height="15.0" fill="rgb(212,35,8)" rx="2" ry="2" />
  691. <text x="415.22" y="479.5" >exc_page_fault</text>
  692. </g>
  693. <g >
  694. <title>_mm512_mask_add_epi64 (1,637,756,210 samples, 3.20%)</title><rect x="952.3" y="469" width="37.7" height="15.0" fill="rgb(246,189,45)" rx="2" ry="2" />
  695. <text x="955.28" y="479.5" >_mm..</text>
  696. </g>
  697. <g >
  698. <title>__handle_mm_fault (7,789,560,264 samples, 15.22%)</title><rect x="415.9" y="421" width="179.5" height="15.0" fill="rgb(207,9,2)" rx="2" ry="2" />
  699. <text x="418.90" y="431.5" >__handle_mm_fault</text>
  700. </g>
  701. <g >
  702. <title>entry_SYSCALL_64_after_hwframe (4,439,475 samples, 0.01%)</title><rect x="1128.2" y="453" width="0.1" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  703. <text x="1131.18" y="463.5" ></text>
  704. </g>
  705. <g >
  706. <title>exit_to_user_mode_prepare (84,694,281 samples, 0.17%)</title><rect x="604.4" y="453" width="2.0" height="15.0" fill="rgb(228,108,25)" rx="2" ry="2" />
  707. <text x="607.41" y="463.5" ></text>
  708. </g>
  709. <g >
  710. <title>charge_memcg (565,367,043 samples, 1.10%)</title><rect x="95.6" y="373" width="13.1" height="15.0" fill="rgb(242,170,40)" rx="2" ry="2" />
  711. <text x="98.64" y="383.5" ></text>
  712. </g>
  713. <g >
  714. <title>__this_cpu_preempt_check (6,027,347 samples, 0.01%)</title><rect x="115.6" y="293" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  715. <text x="118.65" y="303.5" ></text>
  716. </g>
  717. <g >
  718. <title>__x64_sys_get_mempolicy (7,453,000 samples, 0.01%)</title><rect x="1007.5" y="421" width="0.1" height="15.0" fill="rgb(252,217,51)" rx="2" ry="2" />
  719. <text x="1010.47" y="431.5" ></text>
  720. </g>
  721. <g >
  722. <title>cgroup_rstat_updated (10,348,548 samples, 0.02%)</title><rect x="28.1" y="293" width="0.3" height="15.0" fill="rgb(244,180,43)" rx="2" ry="2" />
  723. <text x="31.12" y="303.5" ></text>
  724. </g>
  725. <g >
  726. <title>__do_sys_clone3 (12,937,992 samples, 0.03%)</title><rect x="866.8" y="517" width="0.3" height="15.0" fill="rgb(231,122,29)" rx="2" ry="2" />
  727. <text x="869.82" y="527.5" ></text>
  728. </g>
  729. <g >
  730. <title>irqentry_exit_to_user_mode (41,316,055 samples, 0.08%)</title><rect x="137.5" y="469" width="1.0" height="15.0" fill="rgb(254,229,54)" rx="2" ry="2" />
  731. <text x="140.55" y="479.5" ></text>
  732. </g>
  733. <g >
  734. <title>free_swap_cache (12,071,475 samples, 0.02%)</title><rect x="29.3" y="309" width="0.3" height="15.0" fill="rgb(244,180,43)" rx="2" ry="2" />
  735. <text x="32.27" y="319.5" ></text>
  736. </g>
  737. <g >
  738. <title>tick_sched_handle (7,679,459 samples, 0.02%)</title><rect x="320.8" y="389" width="0.2" height="15.0" fill="rgb(219,68,16)" rx="2" ry="2" />
  739. <text x="323.83" y="399.5" ></text>
  740. </g>
  741. <g >
  742. <title>cgroup_rstat_updated (6,916,629 samples, 0.01%)</title><rect x="596.9" y="389" width="0.1" height="15.0" fill="rgb(244,180,43)" rx="2" ry="2" />
  743. <text x="599.88" y="399.5" ></text>
  744. </g>
  745. <g >
  746. <title>mem_cgroup_charge_statistics (213,849,573 samples, 0.42%)</title><rect x="96.2" y="357" width="5.0" height="15.0" fill="rgb(232,126,30)" rx="2" ry="2" />
  747. <text x="99.24" y="367.5" ></text>
  748. </g>
  749. <g >
  750. <title>dml::submit&lt;dml::hardware, dml::execution_interface&lt;dml::hardware, std::allocator&lt;unsigned char&gt; &gt; &gt; (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="421" width="5.0" height="15.0" fill="rgb(234,134,32)" rx="2" ry="2" />
  751. <text x="1131.30" y="431.5" ></text>
  752. </g>
  753. <g >
  754. <title>handle_mm_fault (29,947,547 samples, 0.06%)</title><rect x="1126.6" y="437" width="0.7" height="15.0" fill="rgb(234,135,32)" rx="2" ry="2" />
  755. <text x="1129.59" y="447.5" ></text>
  756. </g>
  757. <g >
  758. <title>__mod_memcg_lruvec_state (52,719,383 samples, 0.10%)</title><rect x="573.3" y="357" width="1.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  759. <text x="576.33" y="367.5" ></text>
  760. </g>
  761. <g >
  762. <title>__irqentry_text_end (7,779,280 samples, 0.02%)</title><rect x="378.3" y="485" width="0.2" height="15.0" fill="rgb(248,199,47)" rx="2" ry="2" />
  763. <text x="381.32" y="495.5" ></text>
  764. </g>
  765. <g >
  766. <title>__mod_zone_page_state (31,978,239 samples, 0.06%)</title><rect x="567.0" y="325" width="0.8" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  767. <text x="570.04" y="335.5" ></text>
  768. </g>
  769. <g >
  770. <title>_raw_spin_trylock (53,586,323 samples, 0.10%)</title><rect x="587.5" y="325" width="1.3" height="15.0" fill="rgb(222,80,19)" rx="2" ry="2" />
  771. <text x="590.54" y="335.5" ></text>
  772. </g>
  773. <g >
  774. <title>get_mem_cgroup_from_mm (35,627,896 samples, 0.07%)</title><rect x="108.7" y="373" width="0.8" height="15.0" fill="rgb(218,61,14)" rx="2" ry="2" />
  775. <text x="111.67" y="383.5" ></text>
  776. </g>
  777. <g >
  778. <title>lru_gen_add_folio (237,708,968 samples, 0.46%)</title><rect x="562.3" y="341" width="5.5" height="15.0" fill="rgb(216,53,12)" rx="2" ry="2" />
  779. <text x="565.30" y="351.5" ></text>
  780. </g>
  781. <g >
  782. <title>asm_sysvec_apic_timer_interrupt (17,644,723 samples, 0.03%)</title><rect x="1127.7" y="485" width="0.4" height="15.0" fill="rgb(232,127,30)" rx="2" ry="2" />
  783. <text x="1130.66" y="495.5" ></text>
  784. </g>
  785. <g >
  786. <title>perf_adjust_freq_unthr_context (13,548,659 samples, 0.03%)</title><rect x="1127.7" y="325" width="0.3" height="15.0" fill="rgb(236,146,35)" rx="2" ry="2" />
  787. <text x="1130.70" y="335.5" ></text>
  788. </g>
  789. <g >
  790. <title>Sum&lt;unsigned long&gt;::simd_agg (1,637,756,210 samples, 3.20%)</title><rect x="952.3" y="485" width="37.7" height="15.0" fill="rgb(228,107,25)" rx="2" ry="2" />
  791. <text x="955.28" y="495.5" >Sum..</text>
  792. </g>
  793. <g >
  794. <title>device_parse (8,667,141 samples, 0.02%)</title><rect x="1133.3" y="277" width="0.2" height="15.0" fill="rgb(237,147,35)" rx="2" ry="2" />
  795. <text x="1136.31" y="287.5" ></text>
  796. </g>
  797. <g >
  798. <title>__rcu_read_unlock (6,054,769 samples, 0.01%)</title><rect x="413.5" y="437" width="0.1" height="15.0" fill="rgb(253,224,53)" rx="2" ry="2" />
  799. <text x="416.47" y="447.5" ></text>
  800. </g>
  801. <g >
  802. <title>count_memcg_events.constprop.0 (59,357,552 samples, 0.12%)</title><rect x="132.7" y="421" width="1.4" height="15.0" fill="rgb(213,41,9)" rx="2" ry="2" />
  803. <text x="135.72" y="431.5" ></text>
  804. </g>
  805. <g >
  806. <title>cgroup_rstat_updated (9,488,492 samples, 0.02%)</title><rect x="41.8" y="277" width="0.2" height="15.0" fill="rgb(244,180,43)" rx="2" ry="2" />
  807. <text x="44.76" y="287.5" ></text>
  808. </g>
  809. <g >
  810. <title>kmem_cache_alloc_node (5,173,381 samples, 0.01%)</title><rect x="867.0" y="405" width="0.1" height="15.0" fill="rgb(236,142,34)" rx="2" ry="2" />
  811. <text x="869.96" y="415.5" ></text>
  812. </g>
  813. <g >
  814. <title>__rcu_read_unlock (8,769,197 samples, 0.02%)</title><rect x="109.3" y="357" width="0.2" height="15.0" fill="rgb(253,224,53)" rx="2" ry="2" />
  815. <text x="112.29" y="367.5" ></text>
  816. </g>
  817. <g >
  818. <title>pte_alloc_one (10,374,798 samples, 0.02%)</title><rect x="553.3" y="373" width="0.3" height="15.0" fill="rgb(252,217,51)" rx="2" ry="2" />
  819. <text x="556.34" y="383.5" ></text>
  820. </g>
  821. <g >
  822. <title>main (37,159,085,518 samples, 72.58%)</title><rect x="10.4" y="517" width="856.4" height="15.0" fill="rgb(243,179,42)" rx="2" ry="2" />
  823. <text x="13.35" y="527.5" >main</text>
  824. </g>
  825. <g >
  826. <title>do_anonymous_page (28,572,888 samples, 0.06%)</title><rect x="1126.6" y="405" width="0.7" height="15.0" fill="rgb(238,155,37)" rx="2" ry="2" />
  827. <text x="1129.60" y="415.5" ></text>
  828. </g>
  829. <g >
  830. <title>__hrtimer_run_queues (7,679,459 samples, 0.02%)</title><rect x="320.8" y="421" width="0.2" height="15.0" fill="rgb(237,150,35)" rx="2" ry="2" />
  831. <text x="323.83" y="431.5" ></text>
  832. </g>
  833. <g >
  834. <title>__this_cpu_preempt_check (129,647,384 samples, 0.25%)</title><rect x="491.5" y="341" width="3.0" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  835. <text x="494.52" y="351.5" ></text>
  836. </g>
  837. <g >
  838. <title>unsigned long std::uniform_int_distribution&lt;unsigned long&gt;::operator (5,186,627 samples, 0.01%)</title><rect x="1133.9" y="533" width="0.1" height="15.0" fill="rgb(252,216,51)" rx="2" ry="2" />
  839. <text x="1136.89" y="543.5" ></text>
  840. </g>
  841. <g >
  842. <title>check_preemption_disabled (10,346,755 samples, 0.02%)</title><rect x="18.3" y="293" width="0.3" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  843. <text x="21.32" y="303.5" ></text>
  844. </g>
  845. <g >
  846. <title>policy_nodemask (51,791,473 samples, 0.10%)</title><rect x="131.0" y="373" width="1.2" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  847. <text x="133.96" y="383.5" ></text>
  848. </g>
  849. <g >
  850. <title>__rcu_read_unlock (9,312,892 samples, 0.02%)</title><rect x="428.3" y="357" width="0.2" height="15.0" fill="rgb(253,224,53)" rx="2" ry="2" />
  851. <text x="431.31" y="367.5" ></text>
  852. </g>
  853. <g >
  854. <title>mod_lruvec_page_state.constprop.0 (5,186,872 samples, 0.01%)</title><rect x="553.5" y="357" width="0.1" height="15.0" fill="rgb(208,15,3)" rx="2" ry="2" />
  855. <text x="556.46" y="367.5" ></text>
  856. </g>
  857. <g >
  858. <title>__this_cpu_preempt_check (16,355,591 samples, 0.03%)</title><rect x="98.3" y="325" width="0.4" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  859. <text x="101.28" y="335.5" ></text>
  860. </g>
  861. <g >
  862. <title>folio_add_new_anon_rmap (120,552,539 samples, 0.24%)</title><rect x="117.6" y="389" width="2.8" height="15.0" fill="rgb(233,133,31)" rx="2" ry="2" />
  863. <text x="120.58" y="399.5" ></text>
  864. </g>
  865. <g >
  866. <title>__mod_lruvec_state (24,080,793 samples, 0.05%)</title><rect x="115.3" y="325" width="0.6" height="15.0" fill="rgb(226,100,24)" rx="2" ry="2" />
  867. <text x="118.34" y="335.5" ></text>
  868. </g>
  869. <g >
  870. <title>qi_flush_dev_iotlb_pasid (27,592,601 samples, 0.05%)</title><rect x="18.8" y="325" width="0.7" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  871. <text x="21.82" y="335.5" ></text>
  872. </g>
  873. <g >
  874. <title>do_syscall_64 (4,439,475 samples, 0.01%)</title><rect x="1128.2" y="437" width="0.1" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  875. <text x="1131.18" y="447.5" ></text>
  876. </g>
  877. <g >
  878. <title>intel_invalidate_range (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="405" width="0.1" height="15.0" fill="rgb(228,107,25)" rx="2" ry="2" />
  879. <text x="1136.69" y="415.5" ></text>
  880. </g>
  881. <g >
  882. <title>__tlb_remove_page_size (7,761,283 samples, 0.02%)</title><rect x="23.4" y="341" width="0.2" height="15.0" fill="rgb(210,25,6)" rx="2" ry="2" />
  883. <text x="26.41" y="351.5" ></text>
  884. </g>
  885. <g >
  886. <title>pud_val (12,969,218 samples, 0.03%)</title><rect x="595.1" y="405" width="0.3" height="15.0" fill="rgb(238,151,36)" rx="2" ry="2" />
  887. <text x="598.14" y="415.5" ></text>
  888. </g>
  889. <g >
  890. <title>free_pages_and_swap_cache (12,071,475 samples, 0.02%)</title><rect x="29.3" y="325" width="0.3" height="15.0" fill="rgb(222,82,19)" rx="2" ry="2" />
  891. <text x="32.27" y="335.5" ></text>
  892. </g>
  893. <g >
  894. <title>release_pages (24,481,735 samples, 0.05%)</title><rect x="116.8" y="357" width="0.6" height="15.0" fill="rgb(228,106,25)" rx="2" ry="2" />
  895. <text x="119.81" y="367.5" ></text>
  896. </g>
  897. <g >
  898. <title>__mod_lruvec_page_state (82,866,016 samples, 0.16%)</title><rect x="118.4" y="373" width="1.9" height="15.0" fill="rgb(245,185,44)" rx="2" ry="2" />
  899. <text x="121.41" y="383.5" ></text>
  900. </g>
  901. <g >
  902. <title>debug_smp_processor_id (76,082,188 samples, 0.15%)</title><rect x="472.4" y="325" width="1.7" height="15.0" fill="rgb(216,54,12)" rx="2" ry="2" />
  903. <text x="475.38" y="335.5" ></text>
  904. </g>
  905. <g >
  906. <title>qi_submit_sync (27,592,601 samples, 0.05%)</title><rect x="18.8" y="309" width="0.7" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  907. <text x="21.82" y="319.5" ></text>
  908. </g>
  909. <g >
  910. <title>fpregs_assert_state_consistent (21,009,124 samples, 0.04%)</title><rect x="138.0" y="437" width="0.5" height="15.0" fill="rgb(228,109,26)" rx="2" ry="2" />
  911. <text x="141.01" y="447.5" ></text>
  912. </g>
  913. <g >
  914. <title>check_preemption_disabled (19,865,367 samples, 0.04%)</title><rect x="574.1" y="341" width="0.4" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  915. <text x="577.09" y="351.5" ></text>
  916. </g>
  917. <g >
  918. <title>__next_zones_zonelist (59,712,839 samples, 0.12%)</title><rect x="122.8" y="341" width="1.4" height="15.0" fill="rgb(223,86,20)" rx="2" ry="2" />
  919. <text x="125.82" y="351.5" ></text>
  920. </g>
  921. <g >
  922. <title>sum_check (7,506,033,272 samples, 14.66%)</title><rect x="148.0" y="501" width="173.0" height="15.0" fill="rgb(252,218,52)" rx="2" ry="2" />
  923. <text x="151.01" y="511.5" >sum_check</text>
  924. </g>
  925. <g >
  926. <title>sync_regs (716,147,497 samples, 1.40%)</title><rect x="606.4" y="469" width="16.5" height="15.0" fill="rgb(228,106,25)" rx="2" ry="2" />
  927. <text x="609.36" y="479.5" ></text>
  928. </g>
  929. <g >
  930. <title>entry_SYSCALL_64_after_hwframe (1,446,084,556 samples, 2.82%)</title><rect x="10.4" y="485" width="33.3" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  931. <text x="13.35" y="495.5" >en..</text>
  932. </g>
  933. <g >
  934. <title>debug_smp_processor_id (6,049,220 samples, 0.01%)</title><rect x="558.0" y="373" width="0.1" height="15.0" fill="rgb(216,54,12)" rx="2" ry="2" />
  935. <text x="560.96" y="383.5" ></text>
  936. </g>
  937. <g >
  938. <title>__handle_mm_fault (29,086,417 samples, 0.06%)</title><rect x="1126.6" y="421" width="0.7" height="15.0" fill="rgb(207,9,2)" rx="2" ry="2" />
  939. <text x="1129.59" y="431.5" ></text>
  940. </g>
  941. <g >
  942. <title>do_syscall_64 (4,893,850 samples, 0.01%)</title><rect x="1133.3" y="165" width="0.1" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  943. <text x="1136.32" y="175.5" ></text>
  944. </g>
  945. <g >
  946. <title>in_lock_functions (7,782,211 samples, 0.02%)</title><rect x="554.9" y="357" width="0.2" height="15.0" fill="rgb(238,155,37)" rx="2" ry="2" />
  947. <text x="557.87" y="367.5" ></text>
  948. </g>
  949. <g >
  950. <title>perf_iterate_sb.constprop.0 (7,917,062 samples, 0.02%)</title><rect x="147.7" y="357" width="0.2" height="15.0" fill="rgb(229,113,27)" rx="2" ry="2" />
  951. <text x="150.68" y="367.5" ></text>
  952. </g>
  953. <g >
  954. <title>qi_submit_sync (13,797,540 samples, 0.03%)</title><rect x="23.1" y="293" width="0.3" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  955. <text x="26.09" y="303.5" ></text>
  956. </g>
  957. <g >
  958. <title>mtree_range_walk (36,506,379 samples, 0.07%)</title><rect x="135.8" y="405" width="0.8" height="15.0" fill="rgb(215,49,11)" rx="2" ry="2" />
  959. <text x="138.80" y="415.5" ></text>
  960. </g>
  961. <g >
  962. <title>__rmqueue_pcplist (170,232,441 samples, 0.33%)</title><rect x="583.6" y="325" width="3.9" height="15.0" fill="rgb(230,118,28)" rx="2" ry="2" />
  963. <text x="586.61" y="335.5" ></text>
  964. </g>
  965. <g >
  966. <title>Vector_Loader&lt;unsigned long, (744,562,723 samples, 1.45%)</title><rect x="990.0" y="485" width="17.2" height="15.0" fill="rgb(242,170,40)" rx="2" ry="2" />
  967. <text x="993.03" y="495.5" ></text>
  968. </g>
  969. <g >
  970. <title>pmd_page_vaddr (7,779,371 samples, 0.02%)</title><rect x="576.8" y="389" width="0.2" height="15.0" fill="rgb(227,102,24)" rx="2" ry="2" />
  971. <text x="579.84" y="399.5" ></text>
  972. </g>
  973. <g >
  974. <title>__mod_lruvec_page_state (134,523,882 samples, 0.26%)</title><rect x="26.1" y="325" width="3.1" height="15.0" fill="rgb(245,185,44)" rx="2" ry="2" />
  975. <text x="29.05" y="335.5" ></text>
  976. </g>
  977. <g >
  978. <title>memcg_check_events (234,546,968 samples, 0.46%)</title><rect x="101.2" y="357" width="5.4" height="15.0" fill="rgb(206,4,1)" rx="2" ry="2" />
  979. <text x="104.17" y="367.5" ></text>
  980. </g>
  981. <g >
  982. <title>charge_memcg (7,480,344 samples, 0.01%)</title><rect x="1126.6" y="373" width="0.2" height="15.0" fill="rgb(242,170,40)" rx="2" ry="2" />
  983. <text x="1129.60" y="383.5" ></text>
  984. </g>
  985. <g >
  986. <title>entry_SYSCALL_64_after_hwframe (12,937,992 samples, 0.03%)</title><rect x="866.8" y="549" width="0.3" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  987. <text x="869.82" y="559.5" ></text>
  988. </g>
  989. <g >
  990. <title>__GI___mmap64 (14,975,543 samples, 0.03%)</title><rect x="147.6" y="469" width="0.3" height="15.0" fill="rgb(221,77,18)" rx="2" ry="2" />
  991. <text x="150.58" y="479.5" ></text>
  992. </g>
  993. <g >
  994. <title>do_mmap (13,252,429 samples, 0.03%)</title><rect x="147.6" y="405" width="0.3" height="15.0" fill="rgb(228,107,25)" rx="2" ry="2" />
  995. <text x="150.58" y="415.5" ></text>
  996. </g>
  997. <g >
  998. <title>__this_cpu_preempt_check (4,807,293 samples, 0.01%)</title><rect x="100.7" y="341" width="0.1" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  999. <text x="103.73" y="351.5" ></text>
  1000. </g>
  1001. <g >
  1002. <title>__slab_alloc.isra.0 (5,173,381 samples, 0.01%)</title><rect x="867.0" y="389" width="0.1" height="15.0" fill="rgb(205,0,0)" rx="2" ry="2" />
  1003. <text x="869.96" y="399.5" ></text>
  1004. </g>
  1005. <g >
  1006. <title>check_preemption_disabled (13,828,299 samples, 0.03%)</title><rect x="573.0" y="325" width="0.3" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1007. <text x="576.02" y="335.5" ></text>
  1008. </g>
  1009. <g >
  1010. <title>__mmu_notifier_invalidate_range_end (201,181,727 samples, 0.39%)</title><rect x="1128.4" y="101" width="4.7" height="15.0" fill="rgb(207,11,2)" rx="2" ry="2" />
  1011. <text x="1131.43" y="111.5" ></text>
  1012. </g>
  1013. <g >
  1014. <title>__rcu_read_lock (6,913,047 samples, 0.01%)</title><rect x="422.8" y="373" width="0.2" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  1015. <text x="425.83" y="383.5" ></text>
  1016. </g>
  1017. <g >
  1018. <title>perf_event_mmap (5,036,520 samples, 0.01%)</title><rect x="1133.1" y="117" width="0.1" height="15.0" fill="rgb(229,112,26)" rx="2" ry="2" />
  1019. <text x="1136.07" y="127.5" ></text>
  1020. </g>
  1021. <g >
  1022. <title>intel_invalidate_range (69,838,165 samples, 0.14%)</title><rect x="18.8" y="341" width="1.6" height="15.0" fill="rgb(228,107,25)" rx="2" ry="2" />
  1023. <text x="21.82" y="351.5" ></text>
  1024. </g>
  1025. <g >
  1026. <title>dml::detail::ml::impl::hardware::submit (12,752,896 samples, 0.02%)</title><rect x="1133.3" y="405" width="0.3" height="15.0" fill="rgb(234,136,32)" rx="2" ry="2" />
  1027. <text x="1136.26" y="415.5" ></text>
  1028. </g>
  1029. <g >
  1030. <title>__list_add_valid (20,737,220 samples, 0.04%)</title><rect x="586.4" y="309" width="0.4" height="15.0" fill="rgb(211,28,6)" rx="2" ry="2" />
  1031. <text x="589.36" y="319.5" ></text>
  1032. </g>
  1033. <g >
  1034. <title>__mmu_notifier_invalidate_range (18,972,896 samples, 0.04%)</title><rect x="23.0" y="341" width="0.4" height="15.0" fill="rgb(230,115,27)" rx="2" ry="2" />
  1035. <text x="25.97" y="351.5" ></text>
  1036. </g>
  1037. <g >
  1038. <title>entry_SYSCALL_64_after_hwframe (4,893,850 samples, 0.01%)</title><rect x="1133.3" y="181" width="0.1" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  1039. <text x="1136.32" y="191.5" ></text>
  1040. </g>
  1041. <g >
  1042. <title>qi_flush_dev_iotlb_pasid (90,923,354 samples, 0.18%)</title><rect x="1128.4" y="69" width="2.1" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  1043. <text x="1131.43" y="79.5" ></text>
  1044. </g>
  1045. <g >
  1046. <title>__alloc_pages (652,324,426 samples, 1.27%)</title><rect x="578.2" y="357" width="15.1" height="15.0" fill="rgb(233,129,30)" rx="2" ry="2" />
  1047. <text x="581.23" y="367.5" ></text>
  1048. </g>
  1049. <g >
  1050. <title>__free_one_page (58,629,895 samples, 0.11%)</title><rect x="13.9" y="293" width="1.3" height="15.0" fill="rgb(210,25,6)" rx="2" ry="2" />
  1051. <text x="16.89" y="303.5" ></text>
  1052. </g>
  1053. <g >
  1054. <title>__rcu_read_unlock (5,186,301 samples, 0.01%)</title><rect x="562.0" y="341" width="0.1" height="15.0" fill="rgb(253,224,53)" rx="2" ry="2" />
  1055. <text x="565.00" y="351.5" ></text>
  1056. </g>
  1057. <g >
  1058. <title>_raw_spin_unlock (13,824,435 samples, 0.03%)</title><rect x="588.8" y="325" width="0.3" height="15.0" fill="rgb(223,85,20)" rx="2" ry="2" />
  1059. <text x="591.77" y="335.5" ></text>
  1060. </g>
  1061. <g >
  1062. <title>dml::detail::ml::buffer&lt;std::allocator&lt;unsigned char&gt;, dml::detail::descriptor, dml::detail::completion_record&gt;::buffer (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="373" width="5.0" height="15.0" fill="rgb(231,122,29)" rx="2" ry="2" />
  1063. <text x="1131.30" y="383.5" ></text>
  1064. </g>
  1065. <g >
  1066. <title>check_preemption_disabled (14,661,066 samples, 0.03%)</title><rect x="35.2" y="245" width="0.4" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1067. <text x="38.24" y="255.5" ></text>
  1068. </g>
  1069. <g >
  1070. <title>unsigned int std::uniform_int_distribution&lt;unsigned long&gt;::_S_nd&lt;unsigned long, std::mersenne_twister_engine&lt;unsigned long, 32ul, 624ul, 397ul, 31ul, 2567483615ul, 11ul, 4294967295ul, 7ul, 2636928640ul, 15ul, 4022730752ul, 18ul, 1812433253ul&gt;, unsigned int&gt; (7,039,361,847 samples, 13.75%)</title><rect x="704.6" y="453" width="162.2" height="15.0" fill="rgb(237,147,35)" rx="2" ry="2" />
  1071. <text x="707.57" y="463.5" >unsigned int std::un..</text>
  1072. </g>
  1073. <g >
  1074. <title>perf_event_task_tick (13,548,659 samples, 0.03%)</title><rect x="1127.7" y="341" width="0.3" height="15.0" fill="rgb(205,3,0)" rx="2" ry="2" />
  1075. <text x="1130.70" y="351.5" ></text>
  1076. </g>
  1077. <g >
  1078. <title>__list_add_valid (6,899,733 samples, 0.01%)</title><rect x="14.6" y="277" width="0.1" height="15.0" fill="rgb(211,28,6)" rx="2" ry="2" />
  1079. <text x="17.59" y="287.5" ></text>
  1080. </g>
  1081. <g >
  1082. <title>pmd_pfn (8,640,684 samples, 0.02%)</title><rect x="577.0" y="389" width="0.2" height="15.0" fill="rgb(233,129,31)" rx="2" ry="2" />
  1083. <text x="580.02" y="399.5" ></text>
  1084. </g>
  1085. <g >
  1086. <title>intel_invalidate_range (55,187,637 samples, 0.11%)</title><rect x="10.6" y="341" width="1.2" height="15.0" fill="rgb(228,107,25)" rx="2" ry="2" />
  1087. <text x="13.55" y="351.5" ></text>
  1088. </g>
  1089. <g >
  1090. <title>__sysvec_apic_timer_interrupt (16,533,531 samples, 0.03%)</title><rect x="1127.7" y="453" width="0.4" height="15.0" fill="rgb(242,173,41)" rx="2" ry="2" />
  1091. <text x="1130.68" y="463.5" ></text>
  1092. </g>
  1093. <g >
  1094. <title>free_unref_page_commit (26,737,180 samples, 0.05%)</title><rect x="35.9" y="293" width="0.6" height="15.0" fill="rgb(247,196,46)" rx="2" ry="2" />
  1095. <text x="38.87" y="303.5" ></text>
  1096. </g>
  1097. <g >
  1098. <title>update_process_times (7,679,459 samples, 0.02%)</title><rect x="320.8" y="373" width="0.2" height="15.0" fill="rgb(250,209,50)" rx="2" ry="2" />
  1099. <text x="323.83" y="383.5" ></text>
  1100. </g>
  1101. <g >
  1102. <title>sync_regs (372,014,368 samples, 0.73%)</title><rect x="138.5" y="469" width="8.6" height="15.0" fill="rgb(228,106,25)" rx="2" ry="2" />
  1103. <text x="141.50" y="479.5" ></text>
  1104. </g>
  1105. <g >
  1106. <title>check_preemption_disabled (35,439,582 samples, 0.07%)</title><rect x="605.4" y="421" width="0.8" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1107. <text x="608.36" y="431.5" ></text>
  1108. </g>
  1109. <g >
  1110. <title>debug_smp_processor_id (7,778,582 samples, 0.02%)</title><rect x="606.2" y="421" width="0.2" height="15.0" fill="rgb(216,54,12)" rx="2" ry="2" />
  1111. <text x="609.18" y="431.5" ></text>
  1112. </g>
  1113. <g >
  1114. <title>lock_vma_under_rcu (5,682,124 samples, 0.01%)</title><rect x="1127.3" y="437" width="0.1" height="15.0" fill="rgb(251,211,50)" rx="2" ry="2" />
  1115. <text x="1130.28" y="447.5" ></text>
  1116. </g>
  1117. <g >
  1118. <title>unmap_page_range (1,005,492,248 samples, 1.96%)</title><rect x="20.4" y="357" width="23.2" height="15.0" fill="rgb(206,5,1)" rx="2" ry="2" />
  1119. <text x="23.43" y="367.5" >u..</text>
  1120. </g>
  1121. <g >
  1122. <title>auto dml::detail::submit&lt;dml::hardware, dml::mem_copy_operation, dml::execution_interface&lt;dml::hardware, std::allocator&lt;unsigned char&gt; &gt;, dml::submit&lt;dml::hardware, dml::execution_interface&lt;dml::hardware, std::allocator&lt;unsigned char&gt; &gt; &gt; (228,473,295 samples, 0.45%)</title><rect x="1128.3" y="437" width="5.3" height="15.0" fill="rgb(216,53,12)" rx="2" ry="2" />
  1123. <text x="1131.30" y="447.5" ></text>
  1124. </g>
  1125. <g >
  1126. <title>__rcu_read_unlock (11,236,347 samples, 0.02%)</title><rect x="553.1" y="357" width="0.2" height="15.0" fill="rgb(253,224,53)" rx="2" ry="2" />
  1127. <text x="556.08" y="367.5" ></text>
  1128. </g>
  1129. <g >
  1130. <title>dsacache::Cache::ExecuteCopy (228,473,295 samples, 0.45%)</title><rect x="1128.3" y="469" width="5.3" height="15.0" fill="rgb(220,72,17)" rx="2" ry="2" />
  1131. <text x="1131.30" y="479.5" ></text>
  1132. </g>
  1133. <g >
  1134. <title>intel_invalidate_range (201,181,727 samples, 0.39%)</title><rect x="1128.4" y="85" width="4.7" height="15.0" fill="rgb(228,107,25)" rx="2" ry="2" />
  1135. <text x="1131.43" y="95.5" ></text>
  1136. </g>
  1137. <g >
  1138. <title>qi_submit_sync (90,923,354 samples, 0.18%)</title><rect x="1128.4" y="53" width="2.1" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  1139. <text x="1131.43" y="63.5" ></text>
  1140. </g>
  1141. <g >
  1142. <title>__this_cpu_preempt_check (5,333,942 samples, 0.01%)</title><rect x="133.3" y="389" width="0.1" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1143. <text x="136.30" y="399.5" ></text>
  1144. </g>
  1145. <g >
  1146. <title>__free_one_page (122,450,173 samples, 0.24%)</title><rect x="32.8" y="277" width="2.8" height="15.0" fill="rgb(210,25,6)" rx="2" ry="2" />
  1147. <text x="35.75" y="287.5" ></text>
  1148. </g>
  1149. <g >
  1150. <title>folio_add_new_anon_rmap (233,995,661 samples, 0.46%)</title><rect x="569.3" y="389" width="5.4" height="15.0" fill="rgb(233,133,31)" rx="2" ry="2" />
  1151. <text x="572.33" y="399.5" ></text>
  1152. </g>
  1153. <g >
  1154. <title>do_mprotect_pkey (209,389,327 samples, 0.41%)</title><rect x="1128.4" y="149" width="4.9" height="15.0" fill="rgb(252,218,52)" rx="2" ry="2" />
  1155. <text x="1131.43" y="159.5" ></text>
  1156. </g>
  1157. <g >
  1158. <title>policy_nodemask (32,844,665 samples, 0.06%)</title><rect x="593.7" y="373" width="0.7" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  1159. <text x="596.67" y="383.5" ></text>
  1160. </g>
  1161. <g >
  1162. <title>preempt_count_add (6,537,320 samples, 0.01%)</title><rect x="110.4" y="373" width="0.2" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1163. <text x="113.42" y="383.5" ></text>
  1164. </g>
  1165. <g >
  1166. <title>perf_adjust_freq_unthr_context (7,679,459 samples, 0.02%)</title><rect x="320.8" y="325" width="0.2" height="15.0" fill="rgb(236,146,35)" rx="2" ry="2" />
  1167. <text x="323.83" y="335.5" ></text>
  1168. </g>
  1169. <g >
  1170. <title>preempt_count_add (14,697,153 samples, 0.03%)</title><rect x="554.7" y="373" width="0.4" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1171. <text x="557.71" y="383.5" ></text>
  1172. </g>
  1173. <g >
  1174. <title>all (51,196,000,582 samples, 100%)</title><rect x="10.0" y="597" width="1180.0" height="15.0" fill="rgb(213,39,9)" rx="2" ry="2" />
  1175. <text x="13.00" y="607.5" ></text>
  1176. </g>
  1177. <g >
  1178. <title>__list_add_valid (5,175,618 samples, 0.01%)</title><rect x="31.2" y="309" width="0.1" height="15.0" fill="rgb(211,28,6)" rx="2" ry="2" />
  1179. <text x="34.16" y="319.5" ></text>
  1180. </g>
  1181. <g >
  1182. <title>dml::core::dispatcher::hw_dispatcher::hw_dispatcher (11,868,621 samples, 0.02%)</title><rect x="1133.3" y="357" width="0.3" height="15.0" fill="rgb(213,40,9)" rx="2" ry="2" />
  1183. <text x="1136.28" y="367.5" ></text>
  1184. </g>
  1185. <g >
  1186. <title>__irqentry_text_end (8,281,604 samples, 0.02%)</title><rect x="10.1" y="565" width="0.2" height="15.0" fill="rgb(248,199,47)" rx="2" ry="2" />
  1187. <text x="13.11" y="575.5" ></text>
  1188. </g>
  1189. <g >
  1190. <title>lru_gen_add_folio (128,213,280 samples, 0.25%)</title><rect x="113.9" y="341" width="2.9" height="15.0" fill="rgb(216,53,12)" rx="2" ry="2" />
  1191. <text x="116.86" y="351.5" ></text>
  1192. </g>
  1193. <g >
  1194. <title>inc_mm_counter (54,606,929 samples, 0.11%)</title><rect x="120.4" y="389" width="1.2" height="15.0" fill="rgb(238,153,36)" rx="2" ry="2" />
  1195. <text x="123.36" y="399.5" ></text>
  1196. </g>
  1197. <g >
  1198. <title>mtree_range_walk (63,113,187 samples, 0.12%)</title><rect x="601.3" y="405" width="1.5" height="15.0" fill="rgb(215,49,11)" rx="2" ry="2" />
  1199. <text x="604.32" y="415.5" ></text>
  1200. </g>
  1201. <g >
  1202. <title>free_pcppages_bulk (149,181,975 samples, 0.29%)</title><rect x="32.4" y="293" width="3.5" height="15.0" fill="rgb(210,26,6)" rx="2" ry="2" />
  1203. <text x="35.43" y="303.5" ></text>
  1204. </g>
  1205. <g >
  1206. <title>__x64_sys_madvise (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="469" width="0.1" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  1207. <text x="1136.69" y="479.5" ></text>
  1208. </g>
  1209. <g >
  1210. <title>clear_page_erms (81,251,197 samples, 0.16%)</title><rect x="128.6" y="325" width="1.9" height="15.0" fill="rgb(229,113,27)" rx="2" ry="2" />
  1211. <text x="131.61" y="335.5" ></text>
  1212. </g>
  1213. <g >
  1214. <title>irqentry_exit_to_user_mode (90,739,272 samples, 0.18%)</title><rect x="604.3" y="469" width="2.1" height="15.0" fill="rgb(254,229,54)" rx="2" ry="2" />
  1215. <text x="607.27" y="479.5" ></text>
  1216. </g>
  1217. <g >
  1218. <title>folio_add_lru (7,982,057 samples, 0.02%)</title><rect x="1126.8" y="389" width="0.2" height="15.0" fill="rgb(208,17,4)" rx="2" ry="2" />
  1219. <text x="1129.84" y="399.5" ></text>
  1220. </g>
  1221. <g >
  1222. <title>__mod_lruvec_state (65,677,627 samples, 0.13%)</title><rect x="571.8" y="357" width="1.5" height="15.0" fill="rgb(226,100,24)" rx="2" ry="2" />
  1223. <text x="574.82" y="367.5" ></text>
  1224. </g>
  1225. <g >
  1226. <title>__list_del_entry_valid (12,474,939 samples, 0.02%)</title><rect x="127.3" y="309" width="0.3" height="15.0" fill="rgb(239,158,37)" rx="2" ry="2" />
  1227. <text x="130.33" y="319.5" ></text>
  1228. </g>
  1229. <g >
  1230. <title>auto dml::detail::ml::make_mem_move_task&lt;std::allocator&lt;unsigned char&gt; &gt; (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="405" width="5.0" height="15.0" fill="rgb(216,52,12)" rx="2" ry="2" />
  1231. <text x="1131.30" y="415.5" ></text>
  1232. </g>
  1233. <g >
  1234. <title>__count_memcg_events (49,199,350 samples, 0.10%)</title><rect x="133.0" y="405" width="1.1" height="15.0" fill="rgb(250,211,50)" rx="2" ry="2" />
  1235. <text x="135.95" y="415.5" ></text>
  1236. </g>
  1237. <g >
  1238. <title>release_pages (300,901,400 samples, 0.59%)</title><rect x="11.9" y="341" width="6.9" height="15.0" fill="rgb(228,106,25)" rx="2" ry="2" />
  1239. <text x="14.89" y="351.5" ></text>
  1240. </g>
  1241. <g >
  1242. <title>Filter&lt;unsigned long, LT, (5,218,225,108 samples, 10.19%)</title><rect x="1007.8" y="501" width="120.3" height="15.0" fill="rgb(234,136,32)" rx="2" ry="2" />
  1243. <text x="1010.85" y="511.5" >Filter&lt;unsigne..</text>
  1244. </g>
  1245. <g >
  1246. <title>check_preemption_disabled (1,303,282,835 samples, 2.55%)</title><rect x="494.5" y="341" width="30.0" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1247. <text x="497.51" y="351.5" >ch..</text>
  1248. </g>
  1249. <g >
  1250. <title>wqs_init (8,667,141 samples, 0.02%)</title><rect x="1133.3" y="293" width="0.2" height="15.0" fill="rgb(241,169,40)" rx="2" ry="2" />
  1251. <text x="1136.31" y="303.5" ></text>
  1252. </g>
  1253. <g >
  1254. <title>numa_alloc_onnode (18,422,041 samples, 0.04%)</title><rect x="147.6" y="501" width="0.4" height="15.0" fill="rgb(206,8,1)" rx="2" ry="2" />
  1255. <text x="150.58" y="511.5" ></text>
  1256. </g>
  1257. <g >
  1258. <title>__rcu_read_lock (6,542,321 samples, 0.01%)</title><rect x="109.1" y="357" width="0.2" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  1259. <text x="112.13" y="367.5" ></text>
  1260. </g>
  1261. <g >
  1262. <title>__this_cpu_preempt_check (11,209,459 samples, 0.02%)</title><rect x="42.6" y="277" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1263. <text x="45.57" y="287.5" ></text>
  1264. </g>
  1265. <g >
  1266. <title>perf_event_mmap (7,917,062 samples, 0.02%)</title><rect x="147.7" y="373" width="0.2" height="15.0" fill="rgb(229,112,26)" rx="2" ry="2" />
  1267. <text x="150.68" y="383.5" ></text>
  1268. </g>
  1269. <g >
  1270. <title>uncharge_folio (10,349,848 samples, 0.02%)</title><rect x="13.1" y="309" width="0.2" height="15.0" fill="rgb(222,79,19)" rx="2" ry="2" />
  1271. <text x="16.06" y="319.5" ></text>
  1272. </g>
  1273. <g >
  1274. <title>folio_mapping (8,263,496 samples, 0.02%)</title><rect x="113.7" y="341" width="0.2" height="15.0" fill="rgb(248,201,48)" rx="2" ry="2" />
  1275. <text x="116.67" y="351.5" ></text>
  1276. </g>
  1277. <g >
  1278. <title>percpu_counter_add_batch (77,773,726 samples, 0.15%)</title><rect x="574.9" y="373" width="1.8" height="15.0" fill="rgb(241,166,39)" rx="2" ry="2" />
  1279. <text x="577.91" y="383.5" ></text>
  1280. </g>
  1281. <g >
  1282. <title>preempt_count_sub (7,777,329 samples, 0.02%)</title><rect x="588.9" y="309" width="0.2" height="15.0" fill="rgb(240,162,38)" rx="2" ry="2" />
  1283. <text x="591.91" y="319.5" ></text>
  1284. </g>
  1285. <g >
  1286. <title>set_pte (6,053,127 samples, 0.01%)</title><rect x="577.3" y="389" width="0.1" height="15.0" fill="rgb(229,114,27)" rx="2" ry="2" />
  1287. <text x="580.28" y="399.5" ></text>
  1288. </g>
  1289. <g >
  1290. <title>__folio_alloc (377,498,024 samples, 0.74%)</title><rect x="122.0" y="373" width="8.7" height="15.0" fill="rgb(224,91,21)" rx="2" ry="2" />
  1291. <text x="125.03" y="383.5" ></text>
  1292. </g>
  1293. <g >
  1294. <title>__irqentry_text_end (7,399,701 samples, 0.01%)</title><rect x="54.6" y="485" width="0.2" height="15.0" fill="rgb(248,199,47)" rx="2" ry="2" />
  1295. <text x="57.64" y="495.5" ></text>
  1296. </g>
  1297. <g >
  1298. <title>void fill_mt&lt;unsigned long&gt; (23,680,863,101 samples, 46.26%)</title><rect x="321.0" y="501" width="545.8" height="15.0" fill="rgb(206,5,1)" rx="2" ry="2" />
  1299. <text x="324.01" y="511.5" >void fill_mt&lt;unsigned long&gt;</text>
  1300. </g>
  1301. <g >
  1302. <title>__bitmap_intersects (12,103,165 samples, 0.02%)</title><rect x="594.1" y="341" width="0.3" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1303. <text x="597.15" y="351.5" ></text>
  1304. </g>
  1305. <g >
  1306. <title>std::allocator&lt;dml::detail::ml::utils::structure_from&lt;dml::detail::descriptor, dml::detail::completion_record&gt; &gt;::allocate (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="341" width="5.0" height="15.0" fill="rgb(221,76,18)" rx="2" ry="2" />
  1307. <text x="1131.30" y="351.5" ></text>
  1308. </g>
  1309. <g >
  1310. <title>__bitmap_intersects (30,281,058 samples, 0.06%)</title><rect x="131.2" y="357" width="0.7" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1311. <text x="134.16" y="367.5" ></text>
  1312. </g>
  1313. <g >
  1314. <title>check_preemption_disabled (14,451,746 samples, 0.03%)</title><rect x="100.8" y="341" width="0.4" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1315. <text x="103.84" y="351.5" ></text>
  1316. </g>
  1317. <g >
  1318. <title>path_openat (4,455,340 samples, 0.01%)</title><rect x="1133.3" y="101" width="0.1" height="15.0" fill="rgb(249,202,48)" rx="2" ry="2" />
  1319. <text x="1136.32" y="111.5" ></text>
  1320. </g>
  1321. <g >
  1322. <title>lru_gen_del_folio.constprop.0 (126,721,284 samples, 0.25%)</title><rect x="15.9" y="325" width="2.9" height="15.0" fill="rgb(224,91,21)" rx="2" ry="2" />
  1323. <text x="18.90" y="335.5" ></text>
  1324. </g>
  1325. <g >
  1326. <title>__mem_cgroup_uncharge_list (12,937,530 samples, 0.03%)</title><rect x="13.0" y="325" width="0.3" height="15.0" fill="rgb(219,68,16)" rx="2" ry="2" />
  1327. <text x="16.00" y="335.5" ></text>
  1328. </g>
  1329. <g >
  1330. <title>_start (37,160,744,652 samples, 72.59%)</title><rect x="10.3" y="565" width="856.5" height="15.0" fill="rgb(245,185,44)" rx="2" ry="2" />
  1331. <text x="13.32" y="575.5" >_start</text>
  1332. </g>
  1333. <g >
  1334. <title>unmap_region (1,436,595,546 samples, 2.81%)</title><rect x="10.5" y="389" width="33.1" height="15.0" fill="rgb(219,64,15)" rx="2" ry="2" />
  1335. <text x="13.49" y="399.5" >un..</text>
  1336. </g>
  1337. <g >
  1338. <title>exc_page_fault (2,032,313,547 samples, 3.97%)</title><rect x="90.6" y="469" width="46.9" height="15.0" fill="rgb(212,35,8)" rx="2" ry="2" />
  1339. <text x="93.63" y="479.5" >exc_..</text>
  1340. </g>
  1341. <g >
  1342. <title>__mem_cgroup_charge (9,713,896 samples, 0.02%)</title><rect x="1126.6" y="389" width="0.2" height="15.0" fill="rgb(218,60,14)" rx="2" ry="2" />
  1343. <text x="1129.60" y="399.5" ></text>
  1344. </g>
  1345. <g >
  1346. <title>fpregs_assert_state_consistent (43,218,164 samples, 0.08%)</title><rect x="605.4" y="437" width="1.0" height="15.0" fill="rgb(228,109,26)" rx="2" ry="2" />
  1347. <text x="608.36" y="447.5" ></text>
  1348. </g>
  1349. <g >
  1350. <title>__mod_lruvec_state (60,366,886 samples, 0.12%)</title><rect x="26.4" y="309" width="1.3" height="15.0" fill="rgb(226,100,24)" rx="2" ry="2" />
  1351. <text x="29.35" y="319.5" ></text>
  1352. </g>
  1353. <g >
  1354. <title>__list_del_entry_valid (24,208,250 samples, 0.05%)</title><rect x="586.8" y="309" width="0.6" height="15.0" fill="rgb(239,158,37)" rx="2" ry="2" />
  1355. <text x="589.84" y="319.5" ></text>
  1356. </g>
  1357. <g >
  1358. <title>__this_cpu_preempt_check (5,176,133 samples, 0.01%)</title><rect x="35.1" y="245" width="0.1" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1359. <text x="38.12" y="255.5" ></text>
  1360. </g>
  1361. <g >
  1362. <title>do_anonymous_page (7,558,781,189 samples, 14.76%)</title><rect x="420.2" y="405" width="174.2" height="15.0" fill="rgb(238,155,37)" rx="2" ry="2" />
  1363. <text x="423.21" y="415.5" >do_anonymous_page</text>
  1364. </g>
  1365. <g >
  1366. <title>__mod_node_page_state (31,910,261 samples, 0.06%)</title><rect x="40.6" y="277" width="0.7" height="15.0" fill="rgb(213,38,9)" rx="2" ry="2" />
  1367. <text x="43.60" y="287.5" ></text>
  1368. </g>
  1369. <g >
  1370. <title>preempt_count_add (7,776,035 samples, 0.02%)</title><rect x="569.0" y="373" width="0.2" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1371. <text x="572.00" y="383.5" ></text>
  1372. </g>
  1373. <g >
  1374. <title>__bitmap_intersects (7,404,254 samples, 0.01%)</title><rect x="132.0" y="341" width="0.2" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1375. <text x="134.98" y="351.5" ></text>
  1376. </g>
  1377. <g >
  1378. <title>check_preemption_disabled (65,685,265 samples, 0.13%)</title><rect x="475.0" y="341" width="1.5" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1379. <text x="478.03" y="351.5" ></text>
  1380. </g>
  1381. <g >
  1382. <title>asm_exc_page_fault (59,169,480 samples, 0.12%)</title><rect x="1126.3" y="485" width="1.4" height="15.0" fill="rgb(225,93,22)" rx="2" ry="2" />
  1383. <text x="1129.29" y="495.5" ></text>
  1384. </g>
  1385. <g >
  1386. <title>debug_smp_processor_id (764,412,561 samples, 1.49%)</title><rect x="531.1" y="341" width="17.6" height="15.0" fill="rgb(216,54,12)" rx="2" ry="2" />
  1387. <text x="534.10" y="351.5" ></text>
  1388. </g>
  1389. <g >
  1390. <title>do_syscall_64 (1,446,084,556 samples, 2.82%)</title><rect x="10.4" y="469" width="33.3" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  1391. <text x="13.35" y="479.5" >do..</text>
  1392. </g>
  1393. <g >
  1394. <title>folio_batch_move_lru (472,791,106 samples, 0.92%)</title><rect x="558.1" y="373" width="10.9" height="15.0" fill="rgb(207,10,2)" rx="2" ry="2" />
  1395. <text x="561.10" y="383.5" ></text>
  1396. </g>
  1397. <g >
  1398. <title>tick_sched_timer (16,533,531 samples, 0.03%)</title><rect x="1127.7" y="405" width="0.4" height="15.0" fill="rgb(254,227,54)" rx="2" ry="2" />
  1399. <text x="1130.68" y="415.5" ></text>
  1400. </g>
  1401. <g >
  1402. <title>_raw_spin_trylock (29,145,045 samples, 0.06%)</title><rect x="127.7" y="325" width="0.6" height="15.0" fill="rgb(222,80,19)" rx="2" ry="2" />
  1403. <text x="130.66" y="335.5" ></text>
  1404. </g>
  1405. <g >
  1406. <title>folio_add_lru (297,426,407 samples, 0.58%)</title><rect x="110.6" y="389" width="6.9" height="15.0" fill="rgb(208,17,4)" rx="2" ry="2" />
  1407. <text x="113.63" y="399.5" ></text>
  1408. </g>
  1409. <g >
  1410. <title>__rmqueue_pcplist (87,339,301 samples, 0.17%)</title><rect x="125.6" y="325" width="2.1" height="15.0" fill="rgb(230,118,28)" rx="2" ry="2" />
  1411. <text x="128.65" y="335.5" ></text>
  1412. </g>
  1413. <g >
  1414. <title>__folio_alloc (658,377,440 samples, 1.29%)</title><rect x="578.1" y="373" width="15.2" height="15.0" fill="rgb(224,91,21)" rx="2" ry="2" />
  1415. <text x="581.09" y="383.5" ></text>
  1416. </g>
  1417. <g >
  1418. <title>vma_alloc_folio (445,208,498 samples, 0.87%)</title><rect x="121.9" y="389" width="10.3" height="15.0" fill="rgb(245,187,44)" rx="2" ry="2" />
  1419. <text x="124.89" y="399.5" ></text>
  1420. </g>
  1421. <g >
  1422. <title>std::allocator_traits&lt;std::allocator&lt;dml::detail::ml::utils::structure_from&lt;dml::detail::descriptor, dml::detail::completion_record&gt; &gt; &gt;::allocate (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="357" width="5.0" height="15.0" fill="rgb(234,136,32)" rx="2" ry="2" />
  1423. <text x="1131.30" y="367.5" ></text>
  1424. </g>
  1425. <g >
  1426. <title>scan_b (240,991,297 samples, 0.47%)</title><rect x="1128.1" y="517" width="5.6" height="15.0" fill="rgb(247,193,46)" rx="2" ry="2" />
  1427. <text x="1131.12" y="527.5" ></text>
  1428. </g>
  1429. <g >
  1430. <title>cpuset_nodemask_valid_mems_allowed (12,736,238 samples, 0.02%)</title><rect x="131.9" y="357" width="0.3" height="15.0" fill="rgb(233,132,31)" rx="2" ry="2" />
  1431. <text x="134.86" y="367.5" ></text>
  1432. </g>
  1433. <g >
  1434. <title>__split_vma (5,175,874 samples, 0.01%)</title><rect x="10.4" y="389" width="0.1" height="15.0" fill="rgb(237,150,36)" rx="2" ry="2" />
  1435. <text x="13.35" y="399.5" ></text>
  1436. </g>
  1437. <g >
  1438. <title>do_syscall_64 (12,937,992 samples, 0.03%)</title><rect x="866.8" y="533" width="0.3" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  1439. <text x="869.82" y="543.5" ></text>
  1440. </g>
  1441. <g >
  1442. <title>lock_vma_under_rcu (177,202,272 samples, 0.35%)</title><rect x="598.7" y="437" width="4.1" height="15.0" fill="rgb(251,211,50)" rx="2" ry="2" />
  1443. <text x="601.69" y="447.5" ></text>
  1444. </g>
  1445. <g >
  1446. <title>check_preemption_disabled (4,796,679 samples, 0.01%)</title><rect x="115.8" y="293" width="0.1" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1447. <text x="118.79" y="303.5" ></text>
  1448. </g>
  1449. <g >
  1450. <title>dsacache::Cache::SubmitTask (229,070,210 samples, 0.45%)</title><rect x="1128.3" y="485" width="5.3" height="15.0" fill="rgb(236,142,34)" rx="2" ry="2" />
  1451. <text x="1131.29" y="495.5" ></text>
  1452. </g>
  1453. <g >
  1454. <title>__mod_node_page_state (25,394,846 samples, 0.05%)</title><rect x="119.3" y="341" width="0.5" height="15.0" fill="rgb(213,38,9)" rx="2" ry="2" />
  1455. <text x="122.25" y="351.5" ></text>
  1456. </g>
  1457. <g >
  1458. <title>entry_SYSCALL_64_after_hwframe (14,975,543 samples, 0.03%)</title><rect x="147.6" y="453" width="0.3" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  1459. <text x="150.58" y="463.5" ></text>
  1460. </g>
  1461. <g >
  1462. <title>debug_smp_processor_id (8,622,811 samples, 0.02%)</title><rect x="28.9" y="293" width="0.2" height="15.0" fill="rgb(216,54,12)" rx="2" ry="2" />
  1463. <text x="31.90" y="303.5" ></text>
  1464. </g>
  1465. <g >
  1466. <title>handle_mm_fault (1,853,092,701 samples, 3.62%)</title><rect x="91.4" y="437" width="42.7" height="15.0" fill="rgb(234,135,32)" rx="2" ry="2" />
  1467. <text x="94.41" y="447.5" >hand..</text>
  1468. </g>
  1469. <g >
  1470. <title>do_syscall_64 (209,389,327 samples, 0.41%)</title><rect x="1128.4" y="181" width="4.9" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  1471. <text x="1131.43" y="191.5" ></text>
  1472. </g>
  1473. <g >
  1474. <title>count_memcg_events.constprop.0 (132,239,867 samples, 0.26%)</title><rect x="595.6" y="421" width="3.1" height="15.0" fill="rgb(213,41,9)" rx="2" ry="2" />
  1475. <text x="598.62" y="431.5" ></text>
  1476. </g>
  1477. <g >
  1478. <title>std::mersenne_twister_engine&lt;unsigned long, 32ul, 624ul, 397ul, 31ul, 2567483615ul, 11ul, 4294967295ul, 7ul, 2636928640ul, 15ul, 4022730752ul, 18ul, 1812433253ul&gt;::_M_gen_rand (1,754,123,569 samples, 3.43%)</title><rect x="826.4" y="421" width="40.4" height="15.0" fill="rgb(207,12,3)" rx="2" ry="2" />
  1479. <text x="829.39" y="431.5" >std..</text>
  1480. </g>
  1481. <g >
  1482. <title>down_read_trylock (69,146,736 samples, 0.14%)</title><rect x="599.4" y="421" width="1.6" height="15.0" fill="rgb(219,66,15)" rx="2" ry="2" />
  1483. <text x="602.39" y="431.5" ></text>
  1484. </g>
  1485. <g >
  1486. <title>scan_a (5,219,196,992 samples, 10.19%)</title><rect x="1007.8" y="517" width="120.3" height="15.0" fill="rgb(253,223,53)" rx="2" ry="2" />
  1487. <text x="1010.83" y="527.5" >scan_a</text>
  1488. </g>
  1489. <g >
  1490. <title>__mem_cgroup_charge (615,102,235 samples, 1.20%)</title><rect x="95.3" y="389" width="14.2" height="15.0" fill="rgb(218,60,14)" rx="2" ry="2" />
  1491. <text x="98.31" y="399.5" ></text>
  1492. </g>
  1493. <g >
  1494. <title>check_preemption_disabled (19,022,724 samples, 0.04%)</title><rect x="566.5" y="309" width="0.5" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1495. <text x="569.55" y="319.5" ></text>
  1496. </g>
  1497. <g >
  1498. <title>__rcu_read_unlock (6,050,212 samples, 0.01%)</title><rect x="574.6" y="373" width="0.1" height="15.0" fill="rgb(253,224,53)" rx="2" ry="2" />
  1499. <text x="577.59" y="383.5" ></text>
  1500. </g>
  1501. <g >
  1502. <title>__mod_zone_page_state (23,194,936 samples, 0.05%)</title><rect x="116.3" y="325" width="0.5" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  1503. <text x="119.28" y="335.5" ></text>
  1504. </g>
  1505. <g >
  1506. <title>preempt_count_add (8,645,056 samples, 0.02%)</title><rect x="603.7" y="421" width="0.2" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1507. <text x="606.73" y="431.5" ></text>
  1508. </g>
  1509. <g >
  1510. <title>cgroup_rstat_updated (7,782,352 samples, 0.02%)</title><rect x="573.9" y="341" width="0.2" height="15.0" fill="rgb(244,180,43)" rx="2" ry="2" />
  1511. <text x="576.91" y="351.5" ></text>
  1512. </g>
  1513. <g >
  1514. <title>intel_invalidate_range (18,972,896 samples, 0.04%)</title><rect x="23.0" y="325" width="0.4" height="15.0" fill="rgb(228,107,25)" rx="2" ry="2" />
  1515. <text x="25.97" y="335.5" ></text>
  1516. </g>
  1517. <g >
  1518. <title>preempt_count_add (7,910,132 samples, 0.02%)</title><rect x="137.1" y="421" width="0.2" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1519. <text x="140.09" y="431.5" ></text>
  1520. </g>
  1521. <g >
  1522. <title>vma_alloc_folio (5,817,196 samples, 0.01%)</title><rect x="1127.1" y="389" width="0.2" height="15.0" fill="rgb(245,187,44)" rx="2" ry="2" />
  1523. <text x="1130.12" y="399.5" ></text>
  1524. </g>
  1525. <g >
  1526. <title>__x64_sys_munmap (1,442,633,722 samples, 2.82%)</title><rect x="10.4" y="453" width="33.2" height="15.0" fill="rgb(206,7,1)" rx="2" ry="2" />
  1527. <text x="13.35" y="463.5" >__..</text>
  1528. </g>
  1529. <g >
  1530. <title>try_charge_memcg (1,133,283,682 samples, 2.21%)</title><rect x="524.5" y="357" width="26.2" height="15.0" fill="rgb(210,27,6)" rx="2" ry="2" />
  1531. <text x="527.55" y="367.5" >t..</text>
  1532. </g>
  1533. <g >
  1534. <title>exit_to_user_mode_prepare (40,455,338 samples, 0.08%)</title><rect x="137.6" y="453" width="0.9" height="15.0" fill="rgb(228,108,25)" rx="2" ry="2" />
  1535. <text x="140.57" y="463.5" ></text>
  1536. </g>
  1537. <g >
  1538. <title>__mod_node_page_state (51,742,237 samples, 0.10%)</title><rect x="26.6" y="293" width="1.1" height="15.0" fill="rgb(213,38,9)" rx="2" ry="2" />
  1539. <text x="29.55" y="303.5" ></text>
  1540. </g>
  1541. <g >
  1542. <title>perf_event_init_task (9,487,420 samples, 0.02%)</title><rect x="866.9" y="469" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1543. <text x="869.88" y="479.5" ></text>
  1544. </g>
  1545. <g >
  1546. <title>lock_vma_under_rcu (109,438,099 samples, 0.21%)</title><rect x="134.1" y="437" width="2.5" height="15.0" fill="rgb(251,211,50)" rx="2" ry="2" />
  1547. <text x="137.12" y="447.5" ></text>
  1548. </g>
  1549. <g >
  1550. <title>_raw_spin_lock (63,953,100 samples, 0.12%)</title><rect x="553.6" y="389" width="1.5" height="15.0" fill="rgb(239,160,38)" rx="2" ry="2" />
  1551. <text x="556.58" y="399.5" ></text>
  1552. </g>
  1553. <g >
  1554. <title>__mod_memcg_lruvec_state (16,491,655 samples, 0.03%)</title><rect x="115.9" y="325" width="0.4" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1555. <text x="118.90" y="335.5" ></text>
  1556. </g>
  1557. <g >
  1558. <title>check_preemption_disabled (6,896,706 samples, 0.01%)</title><rect x="15.1" y="261" width="0.1" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1559. <text x="18.09" y="271.5" ></text>
  1560. </g>
  1561. <g >
  1562. <title>__alloc_pages (5,187,926 samples, 0.01%)</title><rect x="553.3" y="357" width="0.2" height="15.0" fill="rgb(233,129,30)" rx="2" ry="2" />
  1563. <text x="556.34" y="367.5" ></text>
  1564. </g>
  1565. <g >
  1566. <title>do_madvise (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="453" width="0.1" height="15.0" fill="rgb(224,88,21)" rx="2" ry="2" />
  1567. <text x="1136.69" y="463.5" ></text>
  1568. </g>
  1569. <g >
  1570. <title>__this_cpu_preempt_check (80,379,073 samples, 0.16%)</title><rect x="456.5" y="325" width="1.8" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1571. <text x="459.49" y="335.5" ></text>
  1572. </g>
  1573. <g >
  1574. <title>page_remove_rmap (244,036,722 samples, 0.48%)</title><rect x="23.6" y="341" width="5.7" height="15.0" fill="rgb(252,219,52)" rx="2" ry="2" />
  1575. <text x="26.65" y="351.5" ></text>
  1576. </g>
  1577. <g >
  1578. <title>perf_iterate_sb.constprop.0 (5,036,520 samples, 0.01%)</title><rect x="1133.1" y="101" width="0.1" height="15.0" fill="rgb(229,113,27)" rx="2" ry="2" />
  1579. <text x="1136.07" y="111.5" ></text>
  1580. </g>
  1581. <g >
  1582. <title>main (5,186,627 samples, 0.01%)</title><rect x="1133.9" y="565" width="0.1" height="15.0" fill="rgb(243,179,42)" rx="2" ry="2" />
  1583. <text x="1136.89" y="575.5" ></text>
  1584. </g>
  1585. <g >
  1586. <title>pte_alloc_one (4,825,833 samples, 0.01%)</title><rect x="109.5" y="373" width="0.1" height="15.0" fill="rgb(252,217,51)" rx="2" ry="2" />
  1587. <text x="112.49" y="383.5" ></text>
  1588. </g>
  1589. <g >
  1590. <title>check_preemption_disabled (6,479,558 samples, 0.01%)</title><rect x="119.7" y="325" width="0.1" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1591. <text x="122.69" y="335.5" ></text>
  1592. </g>
  1593. <g >
  1594. <title>release_pages (593,315,450 samples, 1.16%)</title><rect x="29.6" y="325" width="13.6" height="15.0" fill="rgb(228,106,25)" rx="2" ry="2" />
  1595. <text x="32.55" y="335.5" ></text>
  1596. </g>
  1597. <g >
  1598. <title>tick_sched_timer (7,679,459 samples, 0.02%)</title><rect x="320.8" y="405" width="0.2" height="15.0" fill="rgb(254,227,54)" rx="2" ry="2" />
  1599. <text x="323.83" y="415.5" ></text>
  1600. </g>
  1601. <g >
  1602. <title>check_preemption_disabled (70,871,080 samples, 0.14%)</title><rect x="597.0" y="389" width="1.7" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1603. <text x="600.03" y="399.5" ></text>
  1604. </g>
  1605. <g >
  1606. <title>add_wq (8,667,141 samples, 0.02%)</title><rect x="1133.3" y="245" width="0.2" height="15.0" fill="rgb(232,126,30)" rx="2" ry="2" />
  1607. <text x="1136.31" y="255.5" ></text>
  1608. </g>
  1609. <g >
  1610. <title>try_charge_memcg (90,530,113 samples, 0.18%)</title><rect x="106.6" y="357" width="2.1" height="15.0" fill="rgb(210,27,6)" rx="2" ry="2" />
  1611. <text x="109.58" y="367.5" ></text>
  1612. </g>
  1613. <g >
  1614. <title>sysmalloc (211,429,950 samples, 0.41%)</title><rect x="1128.4" y="245" width="4.9" height="15.0" fill="rgb(213,38,9)" rx="2" ry="2" />
  1615. <text x="1131.39" y="255.5" ></text>
  1616. </g>
  1617. <g >
  1618. <title>operator new (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="309" width="5.0" height="15.0" fill="rgb(216,51,12)" rx="2" ry="2" />
  1619. <text x="1131.30" y="319.5" ></text>
  1620. </g>
  1621. <g >
  1622. <title>__mod_memcg_lruvec_state (18,971,182 samples, 0.04%)</title><rect x="18.1" y="309" width="0.5" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1623. <text x="21.14" y="319.5" ></text>
  1624. </g>
  1625. <g >
  1626. <title>do_vmi_align_munmap (1,442,633,722 samples, 2.82%)</title><rect x="10.4" y="405" width="33.2" height="15.0" fill="rgb(211,29,7)" rx="2" ry="2" />
  1627. <text x="13.35" y="415.5" >do..</text>
  1628. </g>
  1629. <g >
  1630. <title>check_preemption_disabled (7,779,084 samples, 0.02%)</title><rect x="576.5" y="357" width="0.2" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1631. <text x="579.52" y="367.5" ></text>
  1632. </g>
  1633. <g >
  1634. <title>vm_mmap_pgoff (14,975,543 samples, 0.03%)</title><rect x="147.6" y="421" width="0.3" height="15.0" fill="rgb(237,150,35)" rx="2" ry="2" />
  1635. <text x="150.58" y="431.5" ></text>
  1636. </g>
  1637. <g >
  1638. <title>__libc_openat64 (4,893,850 samples, 0.01%)</title><rect x="1133.3" y="197" width="0.1" height="15.0" fill="rgb(209,21,5)" rx="2" ry="2" />
  1639. <text x="1136.32" y="207.5" ></text>
  1640. </g>
  1641. <g >
  1642. <title>__mod_lruvec_page_state (157,290,019 samples, 0.31%)</title><rect x="571.0" y="373" width="3.6" height="15.0" fill="rgb(245,185,44)" rx="2" ry="2" />
  1643. <text x="573.96" y="383.5" ></text>
  1644. </g>
  1645. <g >
  1646. <title>check_preemption_disabled (61,772,249 samples, 0.12%)</title><rect x="99.3" y="325" width="1.4" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1647. <text x="102.27" y="335.5" ></text>
  1648. </g>
  1649. <g >
  1650. <title>folio_lruvec_lock_irqsave (6,047,890 samples, 0.01%)</title><rect x="559.4" y="357" width="0.2" height="15.0" fill="rgb(235,138,33)" rx="2" ry="2" />
  1651. <text x="562.41" y="367.5" ></text>
  1652. </g>
  1653. <g >
  1654. <title>dml::core::hardware_device::submit (12,752,896 samples, 0.02%)</title><rect x="1133.3" y="389" width="0.3" height="15.0" fill="rgb(249,202,48)" rx="2" ry="2" />
  1655. <text x="1136.26" y="399.5" ></text>
  1656. </g>
  1657. <g >
  1658. <title>qi_flush_dev_iotlb_pasid (5,175,356 samples, 0.01%)</title><rect x="23.0" y="309" width="0.1" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  1659. <text x="25.97" y="319.5" ></text>
  1660. </g>
  1661. <g >
  1662. <title>qi_flush_piotlb (13,797,540 samples, 0.03%)</title><rect x="23.1" y="309" width="0.3" height="15.0" fill="rgb(251,215,51)" rx="2" ry="2" />
  1663. <text x="26.09" y="319.5" ></text>
  1664. </g>
  1665. <g >
  1666. <title>__this_cpu_preempt_check (10,374,314 samples, 0.02%)</title><rect x="573.7" y="341" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1667. <text x="576.67" y="351.5" ></text>
  1668. </g>
  1669. <g >
  1670. <title>cgroup_rstat_updated (5,188,830 samples, 0.01%)</title><rect x="566.4" y="309" width="0.1" height="15.0" fill="rgb(244,180,43)" rx="2" ry="2" />
  1671. <text x="569.43" y="319.5" ></text>
  1672. </g>
  1673. <g >
  1674. <title>__this_cpu_preempt_check (9,482,915 samples, 0.02%)</title><rect x="27.1" y="277" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1675. <text x="30.07" y="287.5" ></text>
  1676. </g>
  1677. <g >
  1678. <title>__mod_node_page_state (24,198,689 samples, 0.05%)</title><rect x="565.6" y="309" width="0.5" height="15.0" fill="rgb(213,38,9)" rx="2" ry="2" />
  1679. <text x="568.59" y="319.5" ></text>
  1680. </g>
  1681. <g >
  1682. <title>__mod_memcg_lruvec_state (50,024,604 samples, 0.10%)</title><rect x="41.3" y="293" width="1.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1683. <text x="44.34" y="303.5" ></text>
  1684. </g>
  1685. <g >
  1686. <title>tlb_batch_pages_flush (303,488,983 samples, 0.59%)</title><rect x="11.8" y="357" width="7.0" height="15.0" fill="rgb(234,133,32)" rx="2" ry="2" />
  1687. <text x="14.83" y="367.5" ></text>
  1688. </g>
  1689. <g >
  1690. <title>debug_smp_processor_id (6,022,653 samples, 0.01%)</title><rect x="108.2" y="341" width="0.1" height="15.0" fill="rgb(216,54,12)" rx="2" ry="2" />
  1691. <text x="111.19" y="351.5" ></text>
  1692. </g>
  1693. <g >
  1694. <title>__pte_alloc (10,374,798 samples, 0.02%)</title><rect x="553.3" y="389" width="0.3" height="15.0" fill="rgb(218,62,15)" rx="2" ry="2" />
  1695. <text x="556.34" y="399.5" ></text>
  1696. </g>
  1697. <g >
  1698. <title>handle_mm_fault (8,017,729,013 samples, 15.66%)</title><rect x="413.9" y="437" width="184.8" height="15.0" fill="rgb(234,135,32)" rx="2" ry="2" />
  1699. <text x="416.89" y="447.5" >handle_mm_fault</text>
  1700. </g>
  1701. <g >
  1702. <title>accfg_wq_get_first (8,667,141 samples, 0.02%)</title><rect x="1133.3" y="309" width="0.2" height="15.0" fill="rgb(210,26,6)" rx="2" ry="2" />
  1703. <text x="1136.31" y="319.5" ></text>
  1704. </g>
  1705. <g >
  1706. <title>check_preemption_disabled (9,503,613 samples, 0.02%)</title><rect x="565.9" y="293" width="0.2" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1707. <text x="568.93" y="303.5" ></text>
  1708. </g>
  1709. <g >
  1710. <title>__sysvec_apic_timer_interrupt (7,679,459 samples, 0.02%)</title><rect x="320.8" y="453" width="0.2" height="15.0" fill="rgb(242,173,41)" rx="2" ry="2" />
  1711. <text x="323.83" y="463.5" ></text>
  1712. </g>
  1713. <g >
  1714. <title>page_counter_try_charge (82,117,644 samples, 0.16%)</title><rect x="548.7" y="341" width="1.9" height="15.0" fill="rgb(233,132,31)" rx="2" ry="2" />
  1715. <text x="551.72" y="351.5" ></text>
  1716. </g>
  1717. <g >
  1718. <title>__mod_node_page_state (19,093,740 samples, 0.04%)</title><rect x="115.5" y="309" width="0.4" height="15.0" fill="rgb(213,38,9)" rx="2" ry="2" />
  1719. <text x="118.46" y="319.5" ></text>
  1720. </g>
  1721. <g >
  1722. <title>hrtimer_interrupt (16,533,531 samples, 0.03%)</title><rect x="1127.7" y="437" width="0.4" height="15.0" fill="rgb(228,109,26)" rx="2" ry="2" />
  1723. <text x="1130.68" y="447.5" ></text>
  1724. </g>
  1725. <g >
  1726. <title>__this_cpu_preempt_check (5,169,643 samples, 0.01%)</title><rect x="116.4" y="309" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1727. <text x="119.43" y="319.5" ></text>
  1728. </g>
  1729. <g >
  1730. <title>irqentry_enter (6,046,216 samples, 0.01%)</title><rect x="604.0" y="453" width="0.2" height="15.0" fill="rgb(223,84,20)" rx="2" ry="2" />
  1731. <text x="607.03" y="463.5" ></text>
  1732. </g>
  1733. <g >
  1734. <title>preempt_count_add (15,552,403 samples, 0.03%)</title><rect x="588.4" y="309" width="0.4" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1735. <text x="591.41" y="319.5" ></text>
  1736. </g>
  1737. <g >
  1738. <title>zap_page_range_single (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="437" width="0.1" height="15.0" fill="rgb(227,104,24)" rx="2" ry="2" />
  1739. <text x="1136.69" y="447.5" ></text>
  1740. </g>
  1741. <g >
  1742. <title>do_sys_openat2 (4,893,850 samples, 0.01%)</title><rect x="1133.3" y="133" width="0.1" height="15.0" fill="rgb(253,221,52)" rx="2" ry="2" />
  1743. <text x="1136.32" y="143.5" ></text>
  1744. </g>
  1745. <g >
  1746. <title>preempt_count_add (12,102,048 samples, 0.02%)</title><rect x="592.9" y="325" width="0.2" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1747. <text x="595.87" y="335.5" ></text>
  1748. </g>
  1749. <g >
  1750. <title>__mod_lruvec_state (43,985,238 samples, 0.09%)</title><rect x="40.3" y="293" width="1.0" height="15.0" fill="rgb(226,100,24)" rx="2" ry="2" />
  1751. <text x="43.33" y="303.5" ></text>
  1752. </g>
  1753. <g >
  1754. <title>copy_process (12,076,968 samples, 0.02%)</title><rect x="866.8" y="485" width="0.3" height="15.0" fill="rgb(233,130,31)" rx="2" ry="2" />
  1755. <text x="869.82" y="495.5" ></text>
  1756. </g>
  1757. <g >
  1758. <title>lru_add_fn (178,139,222 samples, 0.35%)</title><rect x="112.7" y="357" width="4.1" height="15.0" fill="rgb(208,14,3)" rx="2" ry="2" />
  1759. <text x="115.71" y="367.5" ></text>
  1760. </g>
  1761. <g >
  1762. <title>entry_SYSCALL_64_after_hwframe (10,248,023 samples, 0.02%)</title><rect x="1007.5" y="453" width="0.2" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  1763. <text x="1010.45" y="463.5" ></text>
  1764. </g>
  1765. <g >
  1766. <title>__this_cpu_preempt_check (6,052,056 samples, 0.01%)</title><rect x="572.9" y="325" width="0.1" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1767. <text x="575.88" y="335.5" ></text>
  1768. </g>
  1769. <g >
  1770. <title>do_user_addr_fault (8,304,698,141 samples, 16.22%)</title><rect x="412.6" y="453" width="191.4" height="15.0" fill="rgb(228,108,25)" rx="2" ry="2" />
  1771. <text x="415.62" y="463.5" >do_user_addr_fault</text>
  1772. </g>
  1773. <g >
  1774. <title>__mod_node_page_state (55,310,667 samples, 0.11%)</title><rect x="572.1" y="341" width="1.2" height="15.0" fill="rgb(213,38,9)" rx="2" ry="2" />
  1775. <text x="575.06" y="351.5" ></text>
  1776. </g>
  1777. <g >
  1778. <title>inherit_event.isra.0 (9,487,420 samples, 0.02%)</title><rect x="866.9" y="437" width="0.2" height="15.0" fill="rgb(206,8,2)" rx="2" ry="2" />
  1779. <text x="869.88" y="447.5" ></text>
  1780. </g>
  1781. <g >
  1782. <title>update_process_times (15,726,866 samples, 0.03%)</title><rect x="1127.7" y="373" width="0.4" height="15.0" fill="rgb(250,209,50)" rx="2" ry="2" />
  1783. <text x="1130.70" y="383.5" ></text>
  1784. </g>
  1785. <g >
  1786. <title>_raw_spin_lock (42,338,862 samples, 0.08%)</title><rect x="109.6" y="389" width="1.0" height="15.0" fill="rgb(239,160,38)" rx="2" ry="2" />
  1787. <text x="112.60" y="399.5" ></text>
  1788. </g>
  1789. <g >
  1790. <title>lru_add_fn (356,992,904 samples, 0.70%)</title><rect x="559.6" y="357" width="8.2" height="15.0" fill="rgb(208,14,3)" rx="2" ry="2" />
  1791. <text x="562.55" y="367.5" ></text>
  1792. </g>
  1793. <g >
  1794. <title>qi_flush_piotlb (27,586,822 samples, 0.05%)</title><rect x="11.2" y="325" width="0.6" height="15.0" fill="rgb(251,215,51)" rx="2" ry="2" />
  1795. <text x="14.19" y="335.5" ></text>
  1796. </g>
  1797. <g >
  1798. <title>unsigned long std::uniform_int_distribution&lt;unsigned long&gt;::operator (10,546,449,255 samples, 20.60%)</title><rect x="623.7" y="485" width="243.1" height="15.0" fill="rgb(252,216,51)" rx="2" ry="2" />
  1799. <text x="626.74" y="495.5" >unsigned long std::uniform_int_d..</text>
  1800. </g>
  1801. <g >
  1802. <title>_mm512_stream_load_si512 (744,562,723 samples, 1.45%)</title><rect x="990.0" y="469" width="17.2" height="15.0" fill="rgb(216,52,12)" rx="2" ry="2" />
  1803. <text x="993.03" y="479.5" ></text>
  1804. </g>
  1805. <g >
  1806. <title>entry_SYSCALL_64_after_hwframe (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="501" width="0.1" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  1807. <text x="1136.69" y="511.5" ></text>
  1808. </g>
  1809. <g >
  1810. <title>entry_SYSCALL_64_after_hwframe (209,389,327 samples, 0.41%)</title><rect x="1128.4" y="197" width="4.9" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  1811. <text x="1131.43" y="207.5" ></text>
  1812. </g>
  1813. <g >
  1814. <title>asm_sysvec_apic_timer_interrupt (7,679,459 samples, 0.02%)</title><rect x="320.8" y="485" width="0.2" height="15.0" fill="rgb(232,127,30)" rx="2" ry="2" />
  1815. <text x="323.83" y="495.5" ></text>
  1816. </g>
  1817. <g >
  1818. <title>_mid_memalign (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="293" width="5.0" height="15.0" fill="rgb(218,62,14)" rx="2" ry="2" />
  1819. <text x="1131.30" y="303.5" ></text>
  1820. </g>
  1821. <g >
  1822. <title>preempt_count_add (15,311,608 samples, 0.03%)</title><rect x="135.2" y="405" width="0.3" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1823. <text x="138.19" y="415.5" ></text>
  1824. </g>
  1825. <g >
  1826. <title>__count_memcg_events (106,303,142 samples, 0.21%)</title><rect x="596.2" y="405" width="2.5" height="15.0" fill="rgb(250,211,50)" rx="2" ry="2" />
  1827. <text x="599.22" y="415.5" ></text>
  1828. </g>
  1829. <g >
  1830. <title>preempt_count_add (7,049,342 samples, 0.01%)</title><rect x="130.5" y="325" width="0.2" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1831. <text x="133.50" y="335.5" ></text>
  1832. </g>
  1833. <g >
  1834. <title>preempt_count_add (6,543,516 samples, 0.01%)</title><rect x="128.2" y="309" width="0.1" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1835. <text x="131.18" y="319.5" ></text>
  1836. </g>
  1837. <g >
  1838. <title>__mod_zone_page_state (5,186,354 samples, 0.01%)</title><rect x="587.4" y="309" width="0.1" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  1839. <text x="590.40" y="319.5" ></text>
  1840. </g>
  1841. <g >
  1842. <title>qi_submit_sync (27,600,815 samples, 0.05%)</title><rect x="10.6" y="309" width="0.6" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  1843. <text x="13.55" y="319.5" ></text>
  1844. </g>
  1845. <g >
  1846. <title>dml::detail::ml::task&lt;std::allocator&lt;unsigned char&gt; &gt;::task (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="389" width="5.0" height="15.0" fill="rgb(224,90,21)" rx="2" ry="2" />
  1847. <text x="1131.30" y="399.5" ></text>
  1848. </g>
  1849. <g >
  1850. <title>hrtimer_interrupt (7,679,459 samples, 0.02%)</title><rect x="320.8" y="437" width="0.2" height="15.0" fill="rgb(228,109,26)" rx="2" ry="2" />
  1851. <text x="323.83" y="447.5" ></text>
  1852. </g>
  1853. <g >
  1854. <title>check_preemption_disabled (23,283,575 samples, 0.05%)</title><rect x="28.4" y="293" width="0.5" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1855. <text x="31.36" y="303.5" ></text>
  1856. </g>
  1857. <g >
  1858. <title>accfg_get_param_long (6,285,189 samples, 0.01%)</title><rect x="1133.3" y="229" width="0.2" height="15.0" fill="rgb(217,57,13)" rx="2" ry="2" />
  1859. <text x="1136.31" y="239.5" ></text>
  1860. </g>
  1861. <g >
  1862. <title>__this_cpu_preempt_check (38,903,410 samples, 0.08%)</title><rect x="474.1" y="341" width="0.9" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1863. <text x="477.13" y="351.5" ></text>
  1864. </g>
  1865. <g >
  1866. <title>pmd_val (6,047,707 samples, 0.01%)</title><rect x="595.0" y="405" width="0.1" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  1867. <text x="598.00" y="415.5" ></text>
  1868. </g>
  1869. <g >
  1870. <title>preempt_count_add (13,829,087 samples, 0.03%)</title><rect x="600.6" y="405" width="0.3" height="15.0" fill="rgb(253,222,53)" rx="2" ry="2" />
  1871. <text x="603.60" y="415.5" ></text>
  1872. </g>
  1873. <g >
  1874. <title>tick_sched_handle (15,726,866 samples, 0.03%)</title><rect x="1127.7" y="389" width="0.4" height="15.0" fill="rgb(219,68,16)" rx="2" ry="2" />
  1875. <text x="1130.70" y="399.5" ></text>
  1876. </g>
  1877. <g >
  1878. <title>uncharge_folio (18,971,713 samples, 0.04%)</title><rect x="31.4" y="293" width="0.4" height="15.0" fill="rgb(222,79,19)" rx="2" ry="2" />
  1879. <text x="34.40" y="303.5" ></text>
  1880. </g>
  1881. <g >
  1882. <title>do_syscall_64 (10,248,023 samples, 0.02%)</title><rect x="1007.5" y="437" width="0.2" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  1883. <text x="1010.45" y="447.5" ></text>
  1884. </g>
  1885. <g >
  1886. <title>__list_add_valid (11,210,452 samples, 0.02%)</title><rect x="34.5" y="261" width="0.3" height="15.0" fill="rgb(211,28,6)" rx="2" ry="2" />
  1887. <text x="37.52" y="271.5" ></text>
  1888. </g>
  1889. <g >
  1890. <title>__list_del_entry_valid (12,069,913 samples, 0.02%)</title><rect x="35.6" y="277" width="0.3" height="15.0" fill="rgb(239,158,37)" rx="2" ry="2" />
  1891. <text x="38.57" y="287.5" ></text>
  1892. </g>
  1893. <g >
  1894. <title>__GI_munmap (1,446,084,556 samples, 2.82%)</title><rect x="10.4" y="501" width="33.3" height="15.0" fill="rgb(217,57,13)" rx="2" ry="2" />
  1895. <text x="13.35" y="511.5" >__..</text>
  1896. </g>
  1897. <g >
  1898. <title>std::mersenne_twister_engine&lt;unsigned long, 32ul, 624ul, 397ul, 31ul, 2567483615ul, 11ul, 4294967295ul, 7ul, 2636928640ul, 15ul, 4022730752ul, 18ul, 1812433253ul&gt;::operator (2,429,077,277 samples, 4.74%)</title><rect x="1134.0" y="533" width="56.0" height="15.0" fill="rgb(235,139,33)" rx="2" ry="2" />
  1899. <text x="1137.01" y="543.5" >std::..</text>
  1900. </g>
  1901. <g >
  1902. <title>check_preemption_disabled (19,287,090 samples, 0.04%)</title><rect x="138.0" y="421" width="0.5" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  1903. <text x="141.03" y="431.5" ></text>
  1904. </g>
  1905. <g >
  1906. <title>__mmu_notifier_invalidate_range_end (69,838,165 samples, 0.14%)</title><rect x="18.8" y="357" width="1.6" height="15.0" fill="rgb(207,11,2)" rx="2" ry="2" />
  1907. <text x="21.82" y="367.5" ></text>
  1908. </g>
  1909. <g >
  1910. <title>do_user_addr_fault (2,022,843,060 samples, 3.95%)</title><rect x="90.7" y="453" width="46.6" height="15.0" fill="rgb(228,108,25)" rx="2" ry="2" />
  1911. <text x="93.72" y="463.5" >do_u..</text>
  1912. </g>
  1913. <g >
  1914. <title>__mod_lruvec_state (22,422,367 samples, 0.04%)</title><rect x="17.6" y="309" width="0.5" height="15.0" fill="rgb(226,100,24)" rx="2" ry="2" />
  1915. <text x="20.63" y="319.5" ></text>
  1916. </g>
  1917. <g >
  1918. <title>__rcu_read_unlock (6,045,661 samples, 0.01%)</title><rect x="599.2" y="421" width="0.2" height="15.0" fill="rgb(253,224,53)" rx="2" ry="2" />
  1919. <text x="602.25" y="431.5" ></text>
  1920. </g>
  1921. <g >
  1922. <title>__list_del_entry_valid (7,758,378 samples, 0.02%)</title><rect x="34.8" y="261" width="0.2" height="15.0" fill="rgb(239,158,37)" rx="2" ry="2" />
  1923. <text x="37.78" y="271.5" ></text>
  1924. </g>
  1925. <g >
  1926. <title>__mod_memcg_lruvec_state (38,908,400 samples, 0.08%)</title><rect x="566.1" y="325" width="0.9" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  1927. <text x="569.15" y="335.5" ></text>
  1928. </g>
  1929. <g >
  1930. <title>do_vmi_munmap (1,442,633,722 samples, 2.82%)</title><rect x="10.4" y="421" width="33.2" height="15.0" fill="rgb(253,223,53)" rx="2" ry="2" />
  1931. <text x="13.35" y="431.5" >do..</text>
  1932. </g>
  1933. <g >
  1934. <title>__mod_zone_page_state (16,384,138 samples, 0.03%)</title><rect x="14.9" y="277" width="0.3" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  1935. <text x="17.87" y="287.5" ></text>
  1936. </g>
  1937. <g >
  1938. <title>folio_mapping (7,779,902 samples, 0.02%)</title><rect x="562.1" y="341" width="0.2" height="15.0" fill="rgb(248,201,48)" rx="2" ry="2" />
  1939. <text x="565.12" y="351.5" ></text>
  1940. </g>
  1941. <g >
  1942. <title>__mod_lruvec_state (30,559,640 samples, 0.06%)</title><rect x="119.1" y="357" width="0.7" height="15.0" fill="rgb(226,100,24)" rx="2" ry="2" />
  1943. <text x="122.13" y="367.5" ></text>
  1944. </g>
  1945. <g >
  1946. <title>perf_event_task_tick (7,679,459 samples, 0.02%)</title><rect x="320.8" y="341" width="0.2" height="15.0" fill="rgb(205,3,0)" rx="2" ry="2" />
  1947. <text x="323.83" y="351.5" ></text>
  1948. </g>
  1949. <g >
  1950. <title>mas_walk (43,382,631 samples, 0.08%)</title><rect x="135.6" y="421" width="1.0" height="15.0" fill="rgb(242,170,40)" rx="2" ry="2" />
  1951. <text x="138.64" y="431.5" ></text>
  1952. </g>
  1953. <g >
  1954. <title>numa_node_of_cpu (7,901,696 samples, 0.02%)</title><rect x="1007.3" y="469" width="0.2" height="15.0" fill="rgb(254,227,54)" rx="2" ry="2" />
  1955. <text x="1010.27" y="479.5" ></text>
  1956. </g>
  1957. <g >
  1958. <title>__mod_node_page_state (15,523,973 samples, 0.03%)</title><rect x="17.8" y="293" width="0.3" height="15.0" fill="rgb(213,38,9)" rx="2" ry="2" />
  1959. <text x="20.79" y="303.5" ></text>
  1960. </g>
  1961. <g >
  1962. <title>free_unref_page_list (110,356,941 samples, 0.22%)</title><rect x="13.4" y="325" width="2.5" height="15.0" fill="rgb(221,77,18)" rx="2" ry="2" />
  1963. <text x="16.36" y="335.5" ></text>
  1964. </g>
  1965. <g >
  1966. <title>tlb_batch_pages_flush (605,386,925 samples, 1.18%)</title><rect x="29.3" y="341" width="13.9" height="15.0" fill="rgb(234,133,32)" rx="2" ry="2" />
  1967. <text x="32.27" y="351.5" ></text>
  1968. </g>
  1969. <g >
  1970. <title>openat (4,893,850 samples, 0.01%)</title><rect x="1133.3" y="213" width="0.1" height="15.0" fill="rgb(233,133,31)" rx="2" ry="2" />
  1971. <text x="1136.32" y="223.5" ></text>
  1972. </g>
  1973. <g >
  1974. <title>__mmu_notifier_invalidate_range (55,187,637 samples, 0.11%)</title><rect x="10.6" y="357" width="1.2" height="15.0" fill="rgb(230,115,27)" rx="2" ry="2" />
  1975. <text x="13.55" y="367.5" ></text>
  1976. </g>
  1977. <g >
  1978. <title>error_entry (10,160,085 samples, 0.02%)</title><rect x="90.4" y="469" width="0.2" height="15.0" fill="rgb(240,163,39)" rx="2" ry="2" />
  1979. <text x="93.39" y="479.5" ></text>
  1980. </g>
  1981. <g >
  1982. <title>down_read_trylock (50,243,965 samples, 0.10%)</title><rect x="134.5" y="421" width="1.1" height="15.0" fill="rgb(219,66,15)" rx="2" ry="2" />
  1983. <text x="137.48" y="431.5" ></text>
  1984. </g>
  1985. <g >
  1986. <title>access_error (11,239,905 samples, 0.02%)</title><rect x="413.6" y="437" width="0.3" height="15.0" fill="rgb(227,102,24)" rx="2" ry="2" />
  1987. <text x="416.61" y="447.5" ></text>
  1988. </g>
  1989. <g >
  1990. <title>dsacache::Cache::Access (21,598,768 samples, 0.04%)</title><rect x="1007.3" y="501" width="0.4" height="15.0" fill="rgb(209,18,4)" rx="2" ry="2" />
  1991. <text x="1010.25" y="511.5" ></text>
  1992. </g>
  1993. <g >
  1994. <title>_int_malloc (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="261" width="5.0" height="15.0" fill="rgb(215,47,11)" rx="2" ry="2" />
  1995. <text x="1131.30" y="271.5" ></text>
  1996. </g>
  1997. <g >
  1998. <title>dsacache::Cache::Access (240,484,366 samples, 0.47%)</title><rect x="1128.1" y="501" width="5.6" height="15.0" fill="rgb(209,18,4)" rx="2" ry="2" />
  1999. <text x="1131.12" y="511.5" ></text>
  2000. </g>
  2001. <g >
  2002. <title>_raw_spin_lock (7,702,324 samples, 0.02%)</title><rect x="1132.9" y="37" width="0.1" height="15.0" fill="rgb(239,160,38)" rx="2" ry="2" />
  2003. <text x="1135.87" y="47.5" ></text>
  2004. </g>
  2005. <g >
  2006. <title>__x64_sys_mprotect (209,389,327 samples, 0.41%)</title><rect x="1128.4" y="165" width="4.9" height="15.0" fill="rgb(209,21,5)" rx="2" ry="2" />
  2007. <text x="1131.43" y="175.5" ></text>
  2008. </g>
  2009. <g >
  2010. <title>unsigned long std::uniform_int_distribution&lt;unsigned long&gt;::operator (10,504,101,100 samples, 20.52%)</title><rect x="624.7" y="469" width="242.1" height="15.0" fill="rgb(252,216,51)" rx="2" ry="2" />
  2011. <text x="627.72" y="479.5" >unsigned long std::uniform_int_d..</text>
  2012. </g>
  2013. <g >
  2014. <title>scheduler_tick (7,679,459 samples, 0.02%)</title><rect x="320.8" y="357" width="0.2" height="15.0" fill="rgb(246,190,45)" rx="2" ry="2" />
  2015. <text x="323.83" y="367.5" ></text>
  2016. </g>
  2017. <g >
  2018. <title>qi_submit_sync (5,175,356 samples, 0.01%)</title><rect x="23.0" y="293" width="0.1" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  2019. <text x="25.97" y="303.5" ></text>
  2020. </g>
  2021. <g >
  2022. <title>__GI_mprotect (209,389,327 samples, 0.41%)</title><rect x="1128.4" y="213" width="4.9" height="15.0" fill="rgb(220,71,17)" rx="2" ry="2" />
  2023. <text x="1131.43" y="223.5" ></text>
  2024. </g>
  2025. <g >
  2026. <title>start_thread (11,571,705,609 samples, 22.60%)</title><rect x="867.1" y="549" width="266.7" height="15.0" fill="rgb(212,34,8)" rx="2" ry="2" />
  2027. <text x="870.12" y="559.5" >start_thread</text>
  2028. </g>
  2029. <g >
  2030. <title>check_preemption_disabled (8,062,472 samples, 0.02%)</title><rect x="116.1" y="309" width="0.2" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  2031. <text x="119.07" y="319.5" ></text>
  2032. </g>
  2033. <g >
  2034. <title>check_preemption_disabled (12,102,815 samples, 0.02%)</title><rect x="567.5" y="309" width="0.3" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  2035. <text x="570.50" y="319.5" ></text>
  2036. </g>
  2037. <g >
  2038. <title>__GI_madvise (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="517" width="0.1" height="15.0" fill="rgb(229,113,27)" rx="2" ry="2" />
  2039. <text x="1136.69" y="527.5" ></text>
  2040. </g>
  2041. <g >
  2042. <title>kernel_get_mempolicy (7,453,000 samples, 0.01%)</title><rect x="1007.5" y="405" width="0.1" height="15.0" fill="rgb(229,114,27)" rx="2" ry="2" />
  2043. <text x="1010.47" y="415.5" ></text>
  2044. </g>
  2045. <g >
  2046. <title>kernel_clone (12,937,992 samples, 0.03%)</title><rect x="866.8" y="501" width="0.3" height="15.0" fill="rgb(241,169,40)" rx="2" ry="2" />
  2047. <text x="869.82" y="511.5" ></text>
  2048. </g>
  2049. <g >
  2050. <title>dml::handler&lt;dml::mem_copy_operation, dml::execution_interface&lt;dml::hardware, std::allocator&lt;unsigned char&gt; &gt;::allocator_type&gt; dml::submit&lt;dml::hardware, dml::execution_interface&lt;dml::hardware, std::allocator&lt;unsigned char&gt; &gt; &gt; (228,473,295 samples, 0.45%)</title><rect x="1128.3" y="453" width="5.3" height="15.0" fill="rgb(252,219,52)" rx="2" ry="2" />
  2051. <text x="1131.30" y="463.5" ></text>
  2052. </g>
  2053. <g >
  2054. <title>do_syscall_64 (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="485" width="0.1" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  2055. <text x="1136.69" y="495.5" ></text>
  2056. </g>
  2057. <g >
  2058. <title>[libstdc++.so.6.0.32] (11,565,045,107 samples, 22.59%)</title><rect x="867.1" y="533" width="266.6" height="15.0" fill="rgb(222,81,19)" rx="2" ry="2" />
  2059. <text x="870.12" y="543.5" >[libstdc++.so.6.0.32]</text>
  2060. </g>
  2061. <g >
  2062. <title>free_pcppages_bulk (71,564,161 samples, 0.14%)</title><rect x="13.7" y="309" width="1.6" height="15.0" fill="rgb(210,26,6)" rx="2" ry="2" />
  2063. <text x="16.69" y="319.5" ></text>
  2064. </g>
  2065. <g >
  2066. <title>void fill_mt&lt;unsigned long&gt; (5,186,627 samples, 0.01%)</title><rect x="1133.9" y="549" width="0.1" height="15.0" fill="rgb(206,5,1)" rx="2" ry="2" />
  2067. <text x="1136.89" y="559.5" ></text>
  2068. </g>
  2069. <g >
  2070. <title>percpu_counter_add_batch (50,994,413 samples, 0.10%)</title><rect x="120.4" y="373" width="1.2" height="15.0" fill="rgb(241,166,39)" rx="2" ry="2" />
  2071. <text x="123.44" y="383.5" ></text>
  2072. </g>
  2073. <g >
  2074. <title>free_unref_page_prepare (33,631,349 samples, 0.07%)</title><rect x="36.5" y="293" width="0.8" height="15.0" fill="rgb(238,155,37)" rx="2" ry="2" />
  2075. <text x="39.49" y="303.5" ></text>
  2076. </g>
  2077. <g >
  2078. <title>inherit_task_group.isra.0 (9,487,420 samples, 0.02%)</title><rect x="866.9" y="453" width="0.2" height="15.0" fill="rgb(212,32,7)" rx="2" ry="2" />
  2079. <text x="869.88" y="463.5" ></text>
  2080. </g>
  2081. <g >
  2082. <title>get_page_from_freelist (558,968,342 samples, 1.09%)</title><rect x="580.3" y="341" width="12.9" height="15.0" fill="rgb(252,218,52)" rx="2" ry="2" />
  2083. <text x="583.35" y="351.5" ></text>
  2084. </g>
  2085. <g >
  2086. <title>__mod_zone_page_state (26,737,013 samples, 0.05%)</title><rect x="35.0" y="261" width="0.6" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  2087. <text x="37.96" y="271.5" ></text>
  2088. </g>
  2089. <g >
  2090. <title>access_error (5,680,591 samples, 0.01%)</title><rect x="91.3" y="437" width="0.1" height="15.0" fill="rgb(227,102,24)" rx="2" ry="2" />
  2091. <text x="94.28" y="447.5" ></text>
  2092. </g>
  2093. <g >
  2094. <title>pfn_pte (6,051,666 samples, 0.01%)</title><rect x="576.7" y="389" width="0.1" height="15.0" fill="rgb(231,122,29)" rx="2" ry="2" />
  2095. <text x="579.70" y="399.5" ></text>
  2096. </g>
  2097. <g >
  2098. <title>dml::core::dispatcher::hw_dispatcher::get_instance (11,868,621 samples, 0.02%)</title><rect x="1133.3" y="373" width="0.3" height="15.0" fill="rgb(243,178,42)" rx="2" ry="2" />
  2099. <text x="1136.28" y="383.5" ></text>
  2100. </g>
  2101. <g >
  2102. <title>std::mersenne_twister_engine&lt;unsigned long, 32ul, 624ul, 397ul, 31ul, 2567483615ul, 11ul, 4294967295ul, 7ul, 2636928640ul, 15ul, 4022730752ul, 18ul, 1812433253ul&gt;::operator (3,983,113,625 samples, 7.78%)</title><rect x="775.0" y="437" width="91.8" height="15.0" fill="rgb(235,139,33)" rx="2" ry="2" />
  2103. <text x="778.02" y="447.5" >std::merse..</text>
  2104. </g>
  2105. <g >
  2106. <title>_int_memalign (214,949,728 samples, 0.42%)</title><rect x="1128.3" y="277" width="5.0" height="15.0" fill="rgb(208,17,4)" rx="2" ry="2" />
  2107. <text x="1131.30" y="287.5" ></text>
  2108. </g>
  2109. <g >
  2110. <title>unmap_vmas (1,075,330,413 samples, 2.10%)</title><rect x="18.8" y="373" width="24.8" height="15.0" fill="rgb(243,176,42)" rx="2" ry="2" />
  2111. <text x="21.82" y="383.5" >u..</text>
  2112. </g>
  2113. <g >
  2114. <title>perf_iterate_ctx (5,036,520 samples, 0.01%)</title><rect x="1133.1" y="85" width="0.1" height="15.0" fill="rgb(205,4,0)" rx="2" ry="2" />
  2115. <text x="1136.07" y="95.5" ></text>
  2116. </g>
  2117. <g >
  2118. <title>page_counter_try_charge (13,089,432 samples, 0.03%)</title><rect x="108.3" y="341" width="0.3" height="15.0" fill="rgb(233,132,31)" rx="2" ry="2" />
  2119. <text x="111.33" y="351.5" ></text>
  2120. </g>
  2121. <g >
  2122. <title>check_preemption_disabled (220,193,615 samples, 0.43%)</title><rect x="526.0" y="341" width="5.1" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  2123. <text x="529.02" y="351.5" ></text>
  2124. </g>
  2125. <g >
  2126. <title>cgroup_rstat_updated (26,962,924 samples, 0.05%)</title><rect x="98.7" y="325" width="0.6" height="15.0" fill="rgb(244,180,43)" rx="2" ry="2" />
  2127. <text x="101.65" y="335.5" ></text>
  2128. </g>
  2129. <g >
  2130. <title>pgd_none (7,778,092 samples, 0.02%)</title><rect x="594.7" y="405" width="0.2" height="15.0" fill="rgb(224,88,21)" rx="2" ry="2" />
  2131. <text x="597.72" y="415.5" ></text>
  2132. </g>
  2133. <g >
  2134. <title>qi_submit_sync (110,258,373 samples, 0.22%)</title><rect x="1130.5" y="53" width="2.6" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  2135. <text x="1133.53" y="63.5" ></text>
  2136. </g>
  2137. <g >
  2138. <title>cpuset_nodemask_valid_mems_allowed (16,423,197 samples, 0.03%)</title><rect x="594.0" y="357" width="0.4" height="15.0" fill="rgb(233,132,31)" rx="2" ry="2" />
  2139. <text x="597.05" y="367.5" ></text>
  2140. </g>
  2141. <g >
  2142. <title>qi_flush_piotlb (42,245,564 samples, 0.08%)</title><rect x="19.5" y="325" width="0.9" height="15.0" fill="rgb(251,215,51)" rx="2" ry="2" />
  2143. <text x="22.46" y="335.5" ></text>
  2144. </g>
  2145. <g >
  2146. <title>tlb_finish_mmu (358,676,620 samples, 0.70%)</title><rect x="10.6" y="373" width="8.2" height="15.0" fill="rgb(251,212,50)" rx="2" ry="2" />
  2147. <text x="13.55" y="383.5" ></text>
  2148. </g>
  2149. <g >
  2150. <title>__vm_munmap (1,442,633,722 samples, 2.82%)</title><rect x="10.4" y="437" width="33.2" height="15.0" fill="rgb(231,121,28)" rx="2" ry="2" />
  2151. <text x="13.35" y="447.5" >__..</text>
  2152. </g>
  2153. <g >
  2154. <title>__rcu_read_unlock (6,913,905 samples, 0.01%)</title><rect x="423.0" y="373" width="0.2" height="15.0" fill="rgb(253,224,53)" rx="2" ry="2" />
  2155. <text x="425.99" y="383.5" ></text>
  2156. </g>
  2157. <g >
  2158. <title>__count_memcg_events (1,916,291,637 samples, 3.74%)</title><rect x="430.0" y="341" width="44.1" height="15.0" fill="rgb(250,211,50)" rx="2" ry="2" />
  2159. <text x="432.96" y="351.5" >__co..</text>
  2160. </g>
  2161. <g >
  2162. <title>__mod_zone_page_state (10,350,661 samples, 0.02%)</title><rect x="18.6" y="309" width="0.2" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  2163. <text x="21.58" y="319.5" ></text>
  2164. </g>
  2165. <g >
  2166. <title>pgd_none (4,826,207 samples, 0.01%)</title><rect x="132.2" y="405" width="0.1" height="15.0" fill="rgb(224,88,21)" rx="2" ry="2" />
  2167. <text x="135.15" y="415.5" ></text>
  2168. </g>
  2169. <g >
  2170. <title>mas_walk (77,801,377 samples, 0.15%)</title><rect x="601.0" y="421" width="1.8" height="15.0" fill="rgb(242,170,40)" rx="2" ry="2" />
  2171. <text x="603.98" y="431.5" ></text>
  2172. </g>
  2173. <g >
  2174. <title>qi_flush_piotlb (110,258,373 samples, 0.22%)</title><rect x="1130.5" y="69" width="2.6" height="15.0" fill="rgb(251,215,51)" rx="2" ry="2" />
  2175. <text x="1133.53" y="79.5" ></text>
  2176. </g>
  2177. <g >
  2178. <title>__mod_memcg_lruvec_state (58,635,941 samples, 0.11%)</title><rect x="27.7" y="309" width="1.4" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  2179. <text x="30.74" y="319.5" ></text>
  2180. </g>
  2181. <g >
  2182. <title>clone3 (11,584,643,601 samples, 22.63%)</title><rect x="866.8" y="565" width="267.0" height="15.0" fill="rgb(216,54,12)" rx="2" ry="2" />
  2183. <text x="869.82" y="575.5" >clone3</text>
  2184. </g>
  2185. <g >
  2186. <title>__this_cpu_preempt_check (8,635,064 samples, 0.02%)</title><rect x="567.3" y="309" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  2187. <text x="570.30" y="319.5" ></text>
  2188. </g>
  2189. <g >
  2190. <title>__mem_cgroup_charge (5,673,300,607 samples, 11.08%)</title><rect x="422.6" y="389" width="130.7" height="15.0" fill="rgb(218,60,14)" rx="2" ry="2" />
  2191. <text x="425.58" y="399.5" >__mem_cgroup_cha..</text>
  2192. </g>
  2193. <g >
  2194. <title>__sysfs_device_parse (8,667,141 samples, 0.02%)</title><rect x="1133.3" y="261" width="0.2" height="15.0" fill="rgb(226,99,23)" rx="2" ry="2" />
  2195. <text x="1136.31" y="271.5" ></text>
  2196. </g>
  2197. <g >
  2198. <title>__list_del_entry_valid (6,034,767 samples, 0.01%)</title><rect x="40.2" y="293" width="0.1" height="15.0" fill="rgb(239,158,37)" rx="2" ry="2" />
  2199. <text x="43.19" y="303.5" ></text>
  2200. </g>
  2201. <g >
  2202. <title>policy_node (7,657,304 samples, 0.01%)</title><rect x="130.8" y="373" width="0.2" height="15.0" fill="rgb(236,143,34)" rx="2" ry="2" />
  2203. <text x="133.78" y="383.5" ></text>
  2204. </g>
  2205. <g >
  2206. <title>syscall (4,439,475 samples, 0.01%)</title><rect x="1128.2" y="469" width="0.1" height="15.0" fill="rgb(234,136,32)" rx="2" ry="2" />
  2207. <text x="1131.18" y="479.5" ></text>
  2208. </g>
  2209. <g >
  2210. <title>__libc_start_call_main (37,160,744,652 samples, 72.59%)</title><rect x="10.3" y="533" width="856.5" height="15.0" fill="rgb(210,26,6)" rx="2" ry="2" />
  2211. <text x="13.32" y="543.5" >__libc_start_call_main</text>
  2212. </g>
  2213. <g >
  2214. <title>exc_page_fault (38,214,263 samples, 0.07%)</title><rect x="1126.6" y="469" width="0.9" height="15.0" fill="rgb(212,35,8)" rx="2" ry="2" />
  2215. <text x="1129.59" y="479.5" ></text>
  2216. </g>
  2217. <g >
  2218. <title>dsacache::Cache::SubmitTask (12,752,896 samples, 0.02%)</title><rect x="1133.3" y="421" width="0.3" height="15.0" fill="rgb(236,142,34)" rx="2" ry="2" />
  2219. <text x="1136.26" y="431.5" ></text>
  2220. </g>
  2221. <g >
  2222. <title>check_preemption_disabled (19,837,844 samples, 0.04%)</title><rect x="42.0" y="277" width="0.4" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  2223. <text x="44.98" y="287.5" ></text>
  2224. </g>
  2225. <g >
  2226. <title>__libc_start_main_impl (37,160,744,652 samples, 72.59%)</title><rect x="10.3" y="549" width="856.5" height="15.0" fill="rgb(218,63,15)" rx="2" ry="2" />
  2227. <text x="13.32" y="559.5" >__libc_start_main_impl</text>
  2228. </g>
  2229. <g >
  2230. <title>check_preemption_disabled (17,246,084 samples, 0.03%)</title><rect x="42.8" y="277" width="0.4" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  2231. <text x="45.83" y="287.5" ></text>
  2232. </g>
  2233. <g >
  2234. <title>unsigned int std::uniform_int_distribution&lt;unsigned long&gt;::_S_nd&lt;unsigned long, std::mersenne_twister_engine&lt;unsigned long, 32ul, 624ul, 397ul, 31ul, 2567483615ul, 11ul, 4294967295ul, 7ul, 2636928640ul, 15ul, 4022730752ul, 18ul, 1812433253ul&gt;, unsigned int&gt; (2,429,077,277 samples, 4.74%)</title><rect x="1134.0" y="549" width="56.0" height="15.0" fill="rgb(237,147,35)" rx="2" ry="2" />
  2235. <text x="1137.01" y="559.5" >unsig..</text>
  2236. </g>
  2237. <g >
  2238. <title>__mod_zone_page_state (31,906,268 samples, 0.06%)</title><rect x="42.5" y="293" width="0.7" height="15.0" fill="rgb(221,74,17)" rx="2" ry="2" />
  2239. <text x="45.49" y="303.5" ></text>
  2240. </g>
  2241. <g >
  2242. <title>sysvec_apic_timer_interrupt (16,782,425 samples, 0.03%)</title><rect x="1127.7" y="469" width="0.4" height="15.0" fill="rgb(220,69,16)" rx="2" ry="2" />
  2243. <text x="1130.68" y="479.5" ></text>
  2244. </g>
  2245. <g >
  2246. <title>__this_cpu_preempt_check (8,636,695 samples, 0.02%)</title><rect x="596.7" y="389" width="0.2" height="15.0" fill="rgb(247,195,46)" rx="2" ry="2" />
  2247. <text x="599.68" y="399.5" ></text>
  2248. </g>
  2249. <g >
  2250. <title>unsigned long std::uniform_int_distribution&lt;unsigned long&gt;::operator (2,429,077,277 samples, 4.74%)</title><rect x="1134.0" y="565" width="56.0" height="15.0" fill="rgb(252,216,51)" rx="2" ry="2" />
  2251. <text x="1137.01" y="575.5" >unsig..</text>
  2252. </g>
  2253. <g >
  2254. <title>check_preemption_disabled (19,834,031 samples, 0.04%)</title><rect x="27.3" y="277" width="0.4" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  2255. <text x="30.29" y="287.5" ></text>
  2256. </g>
  2257. <g >
  2258. <title>___slab_alloc (5,173,381 samples, 0.01%)</title><rect x="867.0" y="373" width="0.1" height="15.0" fill="rgb(230,115,27)" rx="2" ry="2" />
  2259. <text x="869.96" y="383.5" ></text>
  2260. </g>
  2261. <g >
  2262. <title>check_preemption_disabled (44,059,020 samples, 0.09%)</title><rect x="107.2" y="341" width="1.0" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  2263. <text x="110.18" y="351.5" ></text>
  2264. </g>
  2265. <g >
  2266. <title>get_page_from_freelist (282,901,670 samples, 0.55%)</title><rect x="124.2" y="341" width="6.5" height="15.0" fill="rgb(252,218,52)" rx="2" ry="2" />
  2267. <text x="127.19" y="351.5" ></text>
  2268. </g>
  2269. <g >
  2270. <title>check_preemption_disabled (8,782,853 samples, 0.02%)</title><rect x="111.6" y="373" width="0.2" height="15.0" fill="rgb(220,73,17)" rx="2" ry="2" />
  2271. <text x="114.63" y="383.5" ></text>
  2272. </g>
  2273. <g >
  2274. <title>__list_del_entry_valid (5,174,842 samples, 0.01%)</title><rect x="14.7" y="277" width="0.2" height="15.0" fill="rgb(239,158,37)" rx="2" ry="2" />
  2275. <text x="17.75" y="287.5" ></text>
  2276. </g>
  2277. <g >
  2278. <title>scheduler_tick (14,864,641 samples, 0.03%)</title><rect x="1127.7" y="357" width="0.3" height="15.0" fill="rgb(246,190,45)" rx="2" ry="2" />
  2279. <text x="1130.70" y="367.5" ></text>
  2280. </g>
  2281. <g >
  2282. <title>pud_val (6,882,155 samples, 0.01%)</title><rect x="132.4" y="405" width="0.2" height="15.0" fill="rgb(238,151,36)" rx="2" ry="2" />
  2283. <text x="135.44" y="415.5" ></text>
  2284. </g>
  2285. <g >
  2286. <title>asm_exc_page_fault (10,602,062,007 samples, 20.71%)</title><rect x="378.5" y="485" width="244.4" height="15.0" fill="rgb(225,93,22)" rx="2" ry="2" />
  2287. <text x="381.50" y="495.5" >asm_exc_page_fault</text>
  2288. </g>
  2289. <g >
  2290. <title>do_syscall_64 (14,975,543 samples, 0.03%)</title><rect x="147.6" y="437" width="0.3" height="15.0" fill="rgb(209,20,4)" rx="2" ry="2" />
  2291. <text x="150.58" y="447.5" ></text>
  2292. </g>
  2293. <g >
  2294. <title>free_unref_page_commit (12,938,068 samples, 0.03%)</title><rect x="15.3" y="309" width="0.3" height="15.0" fill="rgb(247,196,46)" rx="2" ry="2" />
  2295. <text x="18.34" y="319.5" ></text>
  2296. </g>
  2297. <g >
  2298. <title>mem_cgroup_charge_statistics (2,082,259,880 samples, 4.07%)</title><rect x="428.5" y="357" width="48.0" height="15.0" fill="rgb(232,126,30)" rx="2" ry="2" />
  2299. <text x="431.55" y="367.5" >mem_..</text>
  2300. </g>
  2301. <g >
  2302. <title>__mmu_notifier_invalidate_range_end (5,811,133 samples, 0.01%)</title><rect x="1133.7" y="421" width="0.1" height="15.0" fill="rgb(207,11,2)" rx="2" ry="2" />
  2303. <text x="1136.69" y="431.5" ></text>
  2304. </g>
  2305. <g >
  2306. <title>do_anonymous_page (1,641,693,315 samples, 3.21%)</title><rect x="94.3" y="405" width="37.9" height="15.0" fill="rgb(238,155,37)" rx="2" ry="2" />
  2307. <text x="97.32" y="415.5" >do_..</text>
  2308. </g>
  2309. <g >
  2310. <title>__memset_avx512_unaligned_erms (4,505,100,311 samples, 8.80%)</title><rect x="43.7" y="501" width="103.8" height="15.0" fill="rgb(214,43,10)" rx="2" ry="2" />
  2311. <text x="46.68" y="511.5" >__memset_avx..</text>
  2312. </g>
  2313. <g >
  2314. <title>folio_batch_move_lru (237,550,002 samples, 0.46%)</title><rect x="111.9" y="373" width="5.5" height="15.0" fill="rgb(207,10,2)" rx="2" ry="2" />
  2315. <text x="114.90" y="383.5" ></text>
  2316. </g>
  2317. <g >
  2318. <title>qi_submit_sync (27,586,822 samples, 0.05%)</title><rect x="11.2" y="309" width="0.6" height="15.0" fill="rgb(239,159,38)" rx="2" ry="2" />
  2319. <text x="14.19" y="319.5" ></text>
  2320. </g>
  2321. <g >
  2322. <title>sync_regs (7,409,456 samples, 0.01%)</title><rect x="1127.5" y="469" width="0.2" height="15.0" fill="rgb(228,106,25)" rx="2" ry="2" />
  2323. <text x="1130.49" y="479.5" ></text>
  2324. </g>
  2325. <g >
  2326. <title>__list_add_valid (8,625,309 samples, 0.02%)</title><rect x="36.3" y="277" width="0.2" height="15.0" fill="rgb(211,28,6)" rx="2" ry="2" />
  2327. <text x="39.29" y="287.5" ></text>
  2328. </g>
  2329. <g >
  2330. <title>clear_page_erms (156,238,867 samples, 0.31%)</title><rect x="589.2" y="325" width="3.6" height="15.0" fill="rgb(229,113,27)" rx="2" ry="2" />
  2331. <text x="592.17" y="335.5" ></text>
  2332. </g>
  2333. <g >
  2334. <title>__count_memcg_events (180,985,616 samples, 0.35%)</title><rect x="96.6" y="341" width="4.1" height="15.0" fill="rgb(250,211,50)" rx="2" ry="2" />
  2335. <text x="99.56" y="351.5" ></text>
  2336. </g>
  2337. <g >
  2338. <title>error_entry (38,027,670 samples, 0.07%)</title><rect x="622.9" y="485" width="0.8" height="15.0" fill="rgb(240,163,39)" rx="2" ry="2" />
  2339. <text x="625.86" y="495.5" ></text>
  2340. </g>
  2341. <g >
  2342. <title>blk_cgroup_congested (31,984,146 samples, 0.06%)</title><rect x="421.8" y="373" width="0.8" height="15.0" fill="rgb(250,211,50)" rx="2" ry="2" />
  2343. <text x="424.84" y="383.5" ></text>
  2344. </g>
  2345. <g >
  2346. <title>error_entry (28,522,680 samples, 0.06%)</title><rect x="411.6" y="469" width="0.6" height="15.0" fill="rgb(240,163,39)" rx="2" ry="2" />
  2347. <text x="414.56" y="479.5" ></text>
  2348. </g>
  2349. <g >
  2350. <title>irqentry_enter (5,165,357 samples, 0.01%)</title><rect x="137.3" y="453" width="0.2" height="15.0" fill="rgb(223,84,20)" rx="2" ry="2" />
  2351. <text x="140.35" y="463.5" ></text>
  2352. </g>
  2353. <g >
  2354. <title>perf_event_alloc (9,487,420 samples, 0.02%)</title><rect x="866.9" y="421" width="0.2" height="15.0" fill="rgb(209,19,4)" rx="2" ry="2" />
  2355. <text x="869.88" y="431.5" ></text>
  2356. </g>
  2357. <g >
  2358. <title>up_read (30,706,665 samples, 0.06%)</title><rect x="136.6" y="437" width="0.7" height="15.0" fill="rgb(209,18,4)" rx="2" ry="2" />
  2359. <text x="139.64" y="447.5" ></text>
  2360. </g>
  2361. </g>
  2362. </svg>