Chromium Code Reviews
chromiumcodereview-hr@appspot.gserviceaccount.com (chromiumcodereview-hr) | Please choose your nickname with Settings | Help | Chromium Project | Gerrit Changes | Sign out
(1110)

Side by Side Diff: src/opts/SkBlitRow_opts_arm_neon.cpp

Issue 461693004: Let skia build with clang's integrated assembler. (Closed) Base URL: https://chromium.googlesource.com/skia.git@master
Patch Set: . Created 6 years, 4 months ago
Use n/p to move between diff chunks; N/P to move between comments. Draft comments are only viewable by you.
Jump to:
View unified diff | Download patch
« no previous file with comments | « no previous file | src/opts/memset16_neon.S » ('j') | no next file with comments »
Toggle Intra-line Diffs ('i') | Expand Comments ('e') | Collapse Comments ('c') | Show Comments Hide Comments ('s')
OLDNEW
1 /* 1 /*
2 * Copyright 2012 The Android Open Source Project 2 * Copyright 2012 The Android Open Source Project
3 * 3 *
4 * Use of this source code is governed by a BSD-style license that can be 4 * Use of this source code is governed by a BSD-style license that can be
5 * found in the LICENSE file. 5 * found in the LICENSE file.
6 */ 6 */
7 7
8 #include "SkBlitRow_opts_arm_neon.h" 8 #include "SkBlitRow_opts_arm_neon.h"
9 9
10 #include "SkBlitMask.h" 10 #include "SkBlitMask.h"
(...skipping 281 matching lines...) Expand 10 before | Expand all | Expand 10 after
292 "vld1.32 {d1}, [%[src]]! \n\t" 292 "vld1.32 {d1}, [%[src]]! \n\t"
293 293
294 "12: \n\t" 294 "12: \n\t"
295 "tst %[count], #1 \n\t" 295 "tst %[count], #1 \n\t"
296 "beq 11f \n\t" 296 "beq 11f \n\t"
297 "vld1.16 {d24[1]}, [%[dst]]! \n\t" 297 "vld1.16 {d24[1]}, [%[dst]]! \n\t"
298 "vld1.32 {d0[1]}, [%[src]]! \n\t" 298 "vld1.32 {d0[1]}, [%[src]]! \n\t"
299 299
300 "11: \n\t" 300 "11: \n\t"
301 // unzips achieve the same as a vld4 operation 301 // unzips achieve the same as a vld4 operation
302 "vuzpq.u16 q0, q1 \n\t" 302 "vuzp.u16 q0, q1 \n\t"
303 "vuzp.u8 d0, d1 \n\t" 303 "vuzp.u8 d0, d1 \n\t"
304 "vuzp.u8 d2, d3 \n\t" 304 "vuzp.u8 d2, d3 \n\t"
305 // expand 0565 q12 to 8888 {d4-d7} 305 // expand 0565 q12 to 8888 {d4-d7}
306 "vmovn.u16 d4, q12 \n\t" 306 "vmovn.u16 d4, q12 \n\t"
307 "vshr.u16 q11, q12, #5 \n\t" 307 "vshr.u16 q11, q12, #5 \n\t"
308 "vshr.u16 q10, q12, #6+5 \n\t" 308 "vshr.u16 q10, q12, #6+5 \n\t"
309 "vmovn.u16 d5, q11 \n\t" 309 "vmovn.u16 d5, q11 \n\t"
310 "vmovn.u16 d6, q10 \n\t" 310 "vmovn.u16 d6, q10 \n\t"
311 "vshl.u8 d4, d4, #3 \n\t" 311 "vshl.u8 d4, d4, #3 \n\t"
312 "vshl.u8 d5, d5, #2 \n\t" 312 "vshl.u8 d5, d5, #2 \n\t"
(...skipping 1364 matching lines...) Expand 10 before | Expand all | Expand 10 after
1677 S32A_Opaque_BlitRow32_neon_src_alpha, // S32A_Opaque, 1677 S32A_Opaque_BlitRow32_neon_src_alpha, // S32A_Opaque,
1678 #else 1678 #else
1679 S32A_Opaque_BlitRow32_neon, // S32A_Opaque, 1679 S32A_Opaque_BlitRow32_neon, // S32A_Opaque,
1680 #endif 1680 #endif
1681 #ifdef SK_CPU_ARM32 1681 #ifdef SK_CPU_ARM32
1682 S32A_Blend_BlitRow32_neon // S32A_Blend 1682 S32A_Blend_BlitRow32_neon // S32A_Blend
1683 #else 1683 #else
1684 NULL 1684 NULL
1685 #endif 1685 #endif
1686 }; 1686 };
OLDNEW
« no previous file with comments | « no previous file | src/opts/memset16_neon.S » ('j') | no next file with comments »

Powered by Google App Engine
This is Rietveld 408576698