1 /*
2 * Copyright (C) 2015 The Android Open Source Project
3 *
4 * Not a Contribution, Apache license notifications and license are retained
5 * for attribution purposes only.
6 *
7 * Licensed under the Apache License, Version 2.0 (the "License");
8 * you may not use this file except in compliance with the License.
9 * You may obtain a copy of the License at
10 *
11 * http://www.apache.org/licenses/LICENSE-2.0
12 *
13 * Unless required by applicable law or agreed to in writing, software
14 * distributed under the License is distributed on an "AS IS" BASIS,
15 * WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
16 * See the License for the specific language governing permissions and
17 * limitations under the License.
18 */
19
20 #include <stdint.h>
21 #include <malloc.h>
22 #include <arm_neon.h>
23 #include "hwc_delta_panel.h"
24
25 #define BYTE_PER_PIXEL 4
26 #define X_LAST 392
27
28 const static int X_START_TABLE[] = {0,176,168,160,152,152,144,144,136,136,136,128,128,128,120,
29 120,120,112,112,112,112,104,104,104,104,96,96,96,96,96,88,
30 88,88,88,88,80,80,80,80,80,80,72,72,72,72,72,72,64,64,64,64,
31 64,64,64,64,56,56,56,56,56,56,56,48,48,48,48,48,48,48,48,48,
32 40,40,40,40,40,40,40,40,40,40,32,32,32,32,32,32,32,32,32,32,
33 32,32,24,24,24,24,24,24,24,24,24,24,24,24,24,16,16,16,16,16,
34 16,16,16,16,16,16,16,16,16,16,16,16,8,8,8,8,8,8,8,8,8,8,8,8,
35 8,8,8,8,8,8,8,8,8,8,8,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,
36 0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,
37 0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,
38 0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,0,8,
39 8,8,8,8,8,8,8,8,8,8,8,8,8,8,8,8,8,8,8,8,8,8,16,16,16,16,16,
40 16,16,16,16,16,16,16,16,16,16,16,16,24,24,24,24,24,24,24,24,
41 24,24,24,24,24,32,32,32,32,32,32,32,32,32,32,32,32,40,40,40,
42 40,40,40,40,40,40,40,48,48,48,48,48,48,48,48,48,56,56,56,56,
43 56,56,56,64,64,64,64,64,64,64,64,72,72,72,72,72,72,80,80,80,
44 80,80,80,88,88,88,88,88,96,96,96,96,96,104,104,104,104,112,
45 112,112,112,120,120,120,128,128,128,136,136,136,144,144,152,
46 152,160,168,176};
47
48 const static int TABLE_SIZE = sizeof(X_START_TABLE) / sizeof(X_START_TABLE[0]);
49 const static uint8_t MASK[8] = {0xff, 0, 0xff, 0, 0xff, 0, 0xff, 0};
50
51 /*
52 * Delta Real Panel Rending - Delta real pixel rending for Wearable device panel.
53 * pImage - Point to head of display image
54 * width - Input image width
55 * height - Input image height
56 */
deltaPanelRendering(uint8_t * pImage,int width,int height)57 void deltaPanelRendering(uint8_t *pImage, int width, int height)
58 {
59 int x, y;
60 uint8_t *pData;
61 int byteWidth;
62 uint32_t *pPixelAbove, *pPixelCenter, *pPixelBelow, *pPixelEnd;
63 int64_t diff;
64 int xStart, xEnd;
65 const uint8x8_t MASK_8X8 = vld1_u8(MASK);
66 const uint8x8_t THREE_8X8 = vdup_n_u8(3);
67
68 byteWidth = width * BYTE_PER_PIXEL;
69 pData = pImage + byteWidth;
70
71 // center
72 for(y = 1; y < (height - 1) && y < TABLE_SIZE; y++)
73 {
74 xStart = X_START_TABLE[y];
75 xEnd = X_LAST - X_START_TABLE[y];
76 pPixelCenter = ((uint32_t*)pData) + xStart;
77 pPixelEnd = ((uint32_t*)pData) + xEnd;
78 pPixelAbove = pPixelCenter - width;
79 pPixelBelow = pPixelCenter + width;
80
81 // process 8 pixels
82 while (pPixelCenter <= pPixelEnd)
83 {
84 __asm__ __volatile__ (
85 "vld4.8 {d8-d11}, [%[above]]! \n"
86 "vld4.8 {d12-d15}, [%[below]]! \n"
87 "vld4.8 {d16-d19}, [%[center]] \n"
88 #ifdef DELTA_PANEL_R
89 "vbit d12, d8, %[mask] \n"
90 #endif
91 #ifdef DELTA_PANEL_G
92 "vbit d13, d9, %[mask] \n"
93 #endif
94 #ifdef DELTA_PANEL_B
95 "vbit d14, d10, %[mask] \n"
96 #endif
97 #ifdef DELTA_PANEL_R
98 "vmovl.u8 q0, d12 \n"
99 #endif
100 #ifdef DELTA_PANEL_G
101 "vmovl.u8 q1, d13 \n"
102 #endif
103 #ifdef DELTA_PANEL_B
104 "vmovl.u8 q2, d14 \n"
105 #endif
106 #ifdef DELTA_PANEL_R
107 "vmlal.u8 q0, d16, %[three] \n"
108 #endif
109 #ifdef DELTA_PANEL_G
110 "vmlal.u8 q1, d17, %[three] \n"
111 #endif
112 #ifdef DELTA_PANEL_B
113 "vmlal.u8 q2, d18, %[three] \n"
114 #endif
115 #ifdef DELTA_PANEL_R
116 "vshrn.i16 d16, q0, #2 \n"
117 #endif
118 #ifdef DELTA_PANEL_G
119 "vshrn.i16 d17, q1, #2 \n"
120 #endif
121 #ifdef DELTA_PANEL_B
122 "vshrn.i16 d18, q2, #2 \n"
123 #endif
124 "vst4.8 {d16-d19}, [%[center]]! \n"
125 : [above]"+&r"(pPixelAbove)
126 , [below]"+&r"(pPixelBelow)
127 , [center]"+&r"(pPixelCenter)
128 : [mask]"w"(MASK_8X8)
129 , [three]"w"(THREE_8X8)
130 : "d8", "d9", "d10", "d11"
131 , "d12", "d13", "d14", "d15"
132 , "d16", "d17", "d18", "d19"
133 , "q0", "q1", "q2", "memory");
134 }
135
136 pData += byteWidth;
137 }
138 }
139