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

Side by Side Diff: src/core/SkBlitter_RGB16.cpp

Issue 1274873002: Detect MIPS DSP and DSPR2 programattically. (Closed) Base URL: https://skia.googlesource.com/skia.git@master
Patch Set: fold through Created 5 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 | « gyp/common_conditions.gypi ('k') | src/opts/SkBlitRow_opts_mips_dsp.cpp » ('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 2006 The Android Open Source Project 2 * Copyright 2006 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.h" 8 #include "SkBlitRow.h"
9 #include "SkCoreBlitters.h" 9 #include "SkCoreBlitters.h"
10 #include "SkColorPriv.h" 10 #include "SkColorPriv.h"
11 #include "SkDither.h" 11 #include "SkDither.h"
12 #include "SkShader.h" 12 #include "SkShader.h"
13 #include "SkUtils.h" 13 #include "SkUtils.h"
14 #include "SkUtilsArm.h" 14 #include "SkUtilsArm.h"
15 #include "SkXfermode.h" 15 #include "SkXfermode.h"
16 16
17 #if SK_MIPS_HAS_DSP 17 #if defined(__mips_dsp)
18 extern void blitmask_d565_opaque_mips(int width, int height, uint16_t* device, 18 extern void blitmask_d565_opaque_mips(int width, int height, uint16_t* device,
19 unsigned deviceRB, const uint8_t* alpha, 19 unsigned deviceRB, const uint8_t* alpha,
20 uint32_t expanded32, unsigned maskRB); 20 uint32_t expanded32, unsigned maskRB);
21 #endif 21 #endif
22 22
23 #if SK_ARM_NEON_IS_ALWAYS && defined(SK_CPU_LENDIAN) 23 #if SK_ARM_NEON_IS_ALWAYS && defined(SK_CPU_LENDIAN)
24 #include <arm_neon.h> 24 #include <arm_neon.h>
25 extern void SkRGB16BlitterBlitV_neon(uint16_t* device, 25 extern void SkRGB16BlitterBlitV_neon(uint16_t* device,
26 int height, 26 int height,
27 size_t deviceRB, 27 size_t deviceRB,
(...skipping 339 matching lines...) Expand 10 before | Expand all | Expand 10 after
367 if (mask & 0x01) dst[7] = color; \ 367 if (mask & 0x01) dst[7] = color; \
368 } while (0) 368 } while (0)
369 369
370 #define SK_BLITBWMASK_NAME SkRGB16_BlitBW 370 #define SK_BLITBWMASK_NAME SkRGB16_BlitBW
371 #define SK_BLITBWMASK_ARGS , uint16_t color 371 #define SK_BLITBWMASK_ARGS , uint16_t color
372 #define SK_BLITBWMASK_BLIT8(mask, dst) solid_8_pixels(mask, dst, color) 372 #define SK_BLITBWMASK_BLIT8(mask, dst) solid_8_pixels(mask, dst, color)
373 #define SK_BLITBWMASK_GETADDR writable_addr16 373 #define SK_BLITBWMASK_GETADDR writable_addr16
374 #define SK_BLITBWMASK_DEVTYPE uint16_t 374 #define SK_BLITBWMASK_DEVTYPE uint16_t
375 #include "SkBlitBWMaskTemplate.h" 375 #include "SkBlitBWMaskTemplate.h"
376 376
377 #if !defined(SK_MIPS_HAS_DSP) 377 #if !defined(__mips_dsp)
378 static U16CPU blend_compact(uint32_t src32, uint32_t dst32, unsigned scale5) { 378 static U16CPU blend_compact(uint32_t src32, uint32_t dst32, unsigned scale5) {
379 return SkCompact_rgb_16(dst32 + ((src32 - dst32) * scale5 >> 5)); 379 return SkCompact_rgb_16(dst32 + ((src32 - dst32) * scale5 >> 5));
380 } 380 }
381 #endif 381 #endif
382 382
383 void SkRGB16_Opaque_Blitter::blitMask(const SkMask& mask, 383 void SkRGB16_Opaque_Blitter::blitMask(const SkMask& mask,
384 const SkIRect& clip) { 384 const SkIRect& clip) {
385 if (mask.fFormat == SkMask::kBW_Format) { 385 if (mask.fFormat == SkMask::kBW_Format) {
386 SkRGB16_BlitBW(fDevice, mask, clip, fColor16); 386 SkRGB16_BlitBW(fDevice, mask, clip, fColor16);
387 return; 387 return;
(...skipping 70 matching lines...) Expand 10 before | Expand all | Expand 10 after
458 while (w > 0) { 458 while (w > 0) {
459 *device = blend_compact(expanded32, SkExpand_rgb_16(*device), 459 *device = blend_compact(expanded32, SkExpand_rgb_16(*device),
460 SkAlpha255To256(*alpha++) >> 3); 460 SkAlpha255To256(*alpha++) >> 3);
461 device += 1; 461 device += 1;
462 --w; 462 --w;
463 } 463 }
464 device = (uint16_t*)((char*)device + deviceRB); 464 device = (uint16_t*)((char*)device + deviceRB);
465 alpha += maskRB; 465 alpha += maskRB;
466 } while (--height != 0); 466 } while (--height != 0);
467 #undef UNROLL 467 #undef UNROLL
468 #elif SK_MIPS_HAS_DSP 468 #elif defined(__mips_dsp)
469 blitmask_d565_opaque_mips(width, height, device, deviceRB, alpha, expanded32 , maskRB); 469 blitmask_d565_opaque_mips(width, height, device, deviceRB, alpha, expanded32 , maskRB);
470 #else // non-neon code 470 #else // non-neon code
471 do { 471 do {
472 int w = width; 472 int w = width;
473 do { 473 do {
474 *device = blend_compact(expanded32, SkExpand_rgb_16(*device), 474 *device = blend_compact(expanded32, SkExpand_rgb_16(*device),
475 SkAlpha255To256(*alpha++) >> 3); 475 SkAlpha255To256(*alpha++) >> 3);
476 device += 1; 476 device += 1;
477 } while (--w != 0); 477 } while (--w != 0);
478 device = (uint16_t*)((char*)device + deviceRB); 478 device = (uint16_t*)((char*)device + deviceRB);
(...skipping 584 matching lines...) Expand 10 before | Expand all | Expand 10 after
1063 #endif 1063 #endif
1064 } else if (0xFF == SkColorGetA(color)) { 1064 } else if (0xFF == SkColorGetA(color)) {
1065 blitter = allocator->createT<SkRGB16_Opaque_Blitter>(device, paint); 1065 blitter = allocator->createT<SkRGB16_Opaque_Blitter>(device, paint);
1066 } else { 1066 } else {
1067 blitter = allocator->createT<SkRGB16_Blitter>(device, paint); 1067 blitter = allocator->createT<SkRGB16_Blitter>(device, paint);
1068 } 1068 }
1069 } 1069 }
1070 1070
1071 return blitter; 1071 return blitter;
1072 } 1072 }
OLDNEW
« no previous file with comments | « gyp/common_conditions.gypi ('k') | src/opts/SkBlitRow_opts_mips_dsp.cpp » ('j') | no next file with comments »

Powered by Google App Engine
This is Rietveld 408576698