Commit graph

1074652 commits

Author SHA1 Message Date
Jami Kettunen
522ad4866d drm/panel: Add panel driver for Samsung S6E3FC1
The S6E3FC1 is 6" 1080x2160 MIPI DSI command mode AMOLED LCD display
found on OnePlus 5T (2017) smartphones.

The panel needs to be enabled from a device tree using the
"samsung,s6e3fc1" compatible.

This driver was generated using the following & includes some minor
cleanup (such as s/to_s6e3fc1/to_s6e3fc1_panel/g):
$ python3 lmdpdg.py dumpling.dtb -r vddio
2022-03-29 22:52:47 +03:00
Jami Kettunen
7a5876b63a drm/panel: s6e3fa5: Read panel orientation
The panel is mounted upside down on the OnePlus 5, so we need to handle
this in the driver.
2022-03-29 22:52:47 +03:00
Jami Kettunen
2620cc8d7a arm64: dts: msm8998-oneplus-common: Drop unused regulators
Also comment the used ones.
2022-03-29 22:52:47 +03:00
Jami Kettunen
c67fc45041 dt-bindings: display: panel: Document Samsung S6E3FA5 display panel 2022-03-29 22:52:47 +03:00
Jami Kettunen
8bb2d2b6b7 arm64: qcom: msm8998-oneplus-common: Enable NFC 2022-03-29 22:52:47 +03:00
Jami Kettunen
18b60e1e08 drm/panel: Add panel driver for Samsung S6E3FA5
The S6E3FA5 is 5.5" 1080x1920 MIPI DSI command mode AMOLED LCD display
found on OnePlus 5 (2017) smartphones.

The panel needs to be enabled from a device tree using the
"samsung,s6e3fa5" compatible.

This driver was generated using the following & includes some minor
cleanup (such as s/to_s6e3fa5/to_s6e3fa5_panel/g):
$ python3 lmdpdg.py cheeseburger.dtb -r vddio

Signed-off-by: Jami Kettunen <jami.kettunen@protonmail.com>
2022-03-29 22:52:47 +03:00
Jami Kettunen
9f0b72f7d8 [ANNOTATION] Apply some F(x)tec Pro1 patches 2022-03-29 22:52:47 +03:00
Danct12
28a64dcdc1 arm64: dts: msm8998-fxtec-pro1: Add remoteproc configuration 2022-03-29 22:52:47 +03:00
Danct12
9cb6c34719 arm64: dts: msm8998-fxtec-pro1: Enable PMI8998 haptics 2022-03-29 22:52:46 +03:00
Danct12
4c36b04925 arm64: dts: msm8998-fxtec-pro1: Configure PMI8998 fuel gauge
This will account for battery statistics reporting on the Fxtec Pro1 (QX1000)
2022-03-29 22:52:46 +03:00
Jami Kettunen
b800af63dd [ANNOTATION] Apply miscellaneous hacks and patches 2022-03-29 22:52:46 +03:00
Jami Kettunen
af1277a488 module: demote invalid ELF header magic error message to pr_debug
This happens anytime busybox modprobe loads a compressed module and
looks especially ugly on postmarketOS for example (or basically any
initramfs); this error is rather pointless since the module is loaded
anyway afterwards.

Upstream (busybox) has no plans to do anything about this error getting
spammed:
https://www.mail-archive.com/busybox@busybox.net/msg27078.html
2022-03-29 22:52:46 +03:00
Jami Kettunen
1628ae181f ASoC: codecs: tfa989x: Add support for tfa9890
This speaker amp model appears to be rather popular on phones and is
used for example by the OnePlus 5/5T.
2022-03-29 22:52:46 +03:00
Jami Kettunen
51418997ad Input: synaptics-rmi4 - add support for F1A
RMI4 F1A supports the simple capacitive buttons function, it's used for
example on embedded devices such as smartphones for capacitive Android
back and recents buttons.
2022-03-29 22:52:46 +03:00
Jami Kettunen
193be10420 drm/msm: Add A540 device support 2022-03-29 22:52:46 +03:00
Jami Kettunen
bdfeaa075c arm64: dts: qcom: msm8998: add IPA information
Add support for the MSM8998 SoC, which includes IPA version 3.1.
2022-03-29 22:52:46 +03:00
Jami Kettunen
88d6e96419 power: supply: qcom_fg: Report online property 2022-03-29 22:52:46 +03:00
Jami Kettunen
8f429d8978 drm/msm: Mention DSI 10nm PHY support for MSM8998 2022-03-29 22:52:46 +03:00
Jami Kettunen
34121e6055 dt-bindings: Document bindings for all MSM8998 devices 2022-03-29 22:52:46 +03:00
Jami Kettunen
927111b0f5 [HACK] ath10k: Fake MSA ready event after event server arrival
This finally allowed me to get past the 2 ath10k_info()'s in qmi.c!

However, this doesn't fix everything; it seems you *have* to run
diag-router from https://github.com/andersson/diag to calm the firmware
down and stop constantly crashing; need to look into a way to get Wi-Fi
working later without needing this debug crap to be running.
2022-03-29 22:52:46 +03:00
Jami Kettunen
6c3db94d2e [HACK] scripts: Stop appending "+" to localversion
This always gets added and doesn't look nice in the version string, so
it's purely for aesthetic reasons :p
2022-03-29 22:52:46 +03:00
Jami Kettunen
ec6f66ad89 [ANNOTATION] Import WIP "Qualcomm SPMI Fuel Gauge" driver
Drop pmi8994 DTS changes though.

https://gitlab.com/sdm845-mainline/linux/-/commits/driver/pmi8998_fg/
2022-03-29 22:52:46 +03:00
Yassine Oudjana
2eea5fe9f8 power: pmi8998_fg: Rename to qcom_fg and add support for PMI8994/6
This adds support for accessing SRAM. That includes requesting and releasing
access to SRAM by setting some registers and handling the mem-avail IRQ,
configuring access, and reading from/writing to it.

Pre-gen3 fuel gauges require reading from SRAM to get voltage, current
and temperature data. Getting capacity is identical to gen3.

Tested on Xiaomi Mi Note 2 with PMI8996.
2022-03-29 22:52:46 +03:00
Yassine Oudjana
87e5901e2b power: pmi8998_fg: Remove some trailing spaces and tabs
This should be squashed.
2022-03-29 22:52:46 +03:00
Joel Selvaraj
fff3a97cdc arm64: dts: qcom: sdm845-oneplus: enable pmi8998 fuel guage
Enable the new pmi8998 fuel gauge

Signed-off-by: Caleb Connolly <caleb@connolly.tech>
2022-03-29 22:52:46 +03:00
Joel Selvaraj
f1b6077a13 fg: clean and read charge full and max voltage from dts 2022-03-29 22:52:45 +03:00
Joel Selvaraj
d962bb5d78 power: supply: add battery charging status feature 2022-03-29 22:52:45 +03:00
Joel Selvaraj
8a66c540f2 arm64: dts: qcom: pmi8998: Add nodes for pmi8998 fuel guage 2022-03-29 22:52:45 +03:00
Joel Selvaraj
0c7a8ce70a power: supply: introduce pmi8998 fuel guage driver 2022-03-29 22:52:45 +03:00
Jami Kettunen
f780d839de [ANNOTATION] Import SPMI haptics driver v4
Drop SDM845 DTS changes though.

Link: https://patchwork.kernel.org/project/linux-arm-msm/cover/20211210022639.2779173-1-caleb@connolly.tech/
2022-03-29 22:52:45 +03:00
Jami Kettunen
6f6f039c9e arm64: dts: qcom: msm8998-oneplus-common: Enable PMI8998 haptics
The OnePlus 5 and 5T both have a haptics engine connected to PMI8998.

Signed-off-by: Jami Kettunen <jami.kettunen@somainline.org>
Signed-off-by: Caleb Connolly <caleb@connolly.tech>
2022-03-29 22:52:45 +03:00
Caleb Connolly
e20414070b arm64: dts: qcom: pmi8998: introduce spmi haptics
Add bindings for Qualcomm SPMI haptics on platforms using pmi8998.

Signed-off-by: Caleb Connolly <caleb@connolly.tech>
2022-03-29 22:52:45 +03:00
Caleb Connolly
769df9c28b input: add Qualcomm SPMI haptics driver
Add support for the haptics found in pmi8998 and related PMICs.
Based on the ff-memless interface. Currently this driver provides
a partial implementation of hardware features.

This driver only supports LRAs (Linear Resonant Actuators) in the "buffer"
mode with a single wave pattern.

Signed-off-by: Caleb Connolly <caleb@connolly.tech>
2022-03-29 22:52:45 +03:00
Caleb Connolly
61491d1901 dt-bindings: input: add Qualcomm SPMI haptics driver
Add bindings for qcom PMIC SPMI haptics driver.

Signed-off-by: Caleb Connolly <caleb@connolly.tech>
2022-03-29 22:52:45 +03:00
Jami Kettunen
c53aa1d6d4 [ANNOTATION] Base @ angelo/5.14-msm8998-audio-working
I also rebased this tree on the linus/v5.17-rc1 tag and while at it
finally dropped changes irrelevant to msm8998.
2022-03-29 22:52:45 +03:00
AngeloGioacchino Del Regno
e3fa3e3ed1 adreno 5xx: TTBR1 extravaganza on MSM8998
(JAMI: fixup for 5.16)
2022-03-29 22:52:45 +03:00
Jami Kettunen
0b49adafb0 arm64: dts: qcom: msm8998-xperia: various tests
Originally from: c215a022
2022-03-29 22:52:45 +03:00
Jami Kettunen
5b33bb9362 ASoC: wcd9335: various tests
Originally from: c215a022
2022-03-29 22:52:45 +03:00
AngeloGioacchino Del Regno
0bc0889e02 iommu/arm-smmu-qcom: Add MSM8998 and SDM660 mss compatibles for identity
Add MSM8998 and SDM660's mss-pil compatibles to switch the default
iommu domain type to IDENTITY, as similarly required by SDM845 and
others.

Signed-off-by: AngeloGioacchino Del Regno <angelogioacchino.delregno@somainline.org>
2022-03-29 22:52:45 +03:00
AngeloGioacchino Del Regno
ed0bb1af2a iommu/arm-smmu-qcom: Skip the TTBR1 quirk for MSM8998 and SDM630
Similarly to MSM8996 DragonBoard 820c, MSM8998 and SDM630 are equipped
with Adreno 5xx series, which doesn't have separate pagetables support
at the moment of writing.
Skip the TTBR1 quirk for these two SoCs as to get Adreno in a usable
state.
2022-03-29 22:52:45 +03:00
AngeloGioacchino Del Regno
ed8cdf8803 arm64: dts: qcom: AUDIO WORKS oon MSM8998 Sony Yoshino platform!!! 2022-03-29 22:52:45 +03:00
AngeloGioacchino Del Regno
306b319190 ASoC: codecs: wcd9335: Fix headphone jack commit for new upstream kernel 2022-03-29 22:52:45 +03:00
Srinivas Kandagatla
b908c27f65 ASoC: wcd9335: add mbhc support
Signed-off-by: Srinivas Kandagatla <srinivas.kandagatla@linaro.org>
2022-03-29 22:52:45 +03:00
Jami Kettunen
c5da981db7 arm64: dts: qcom: Enable audio on MSM8998 Sony Yoshino platform
Originally from: d95b982a
2022-03-29 22:52:44 +03:00
Jami Kettunen
be48c36833 arm64: dts: qcom: msm8998: More audio related node changes
Originally from: d95b982a
2022-03-29 22:52:44 +03:00
Jami Kettunen
e7f46aaebe fixup! arm64: dts: qcom: msm8998: Configure Adreno GPU and related IOMMU 2022-03-29 22:52:44 +03:00
Jami Kettunen
ddb5a4ec04 mfd: wcd9335: Add support to wcd9335 codec
Qualcomm WCD9335 Codec is a standalone Hi-Fi audio codec IC.

This codec has integrated SoundWire controller, pin controller and
interrupt controller.

Originally from: d95b982a
2022-03-29 22:52:44 +03:00
AngeloGioacchino Del Regno
2a698c43a6 arm64: dts: qcom: msm8998: Add disabled slimbus support
Add generic slimbus configuration to MSM8998 and keep it disabled.
It is expected that this will be enabled in board-specific device
trees when supported, along with the right audio codec.

Signed-off-by: AngeloGioacchino Del Regno <angelogioacchino.delregno@somainline.org>
2022-03-29 22:52:44 +03:00
Jami Kettunen
27d473117b ASoC: qcom: lpass-msm8998: Add platform driver for lpass audio
Add platform driver for configuring msm8998 lpass core I2S and
DMA configuration to support playback & capture to external codecs
connected over primary & secondary MI2S interfaces.

(driver originally split from 4d7e1ead3b ("fastmatrix yaml fix"))
2022-03-29 22:52:44 +03:00
AngeloGioacchino Del Regno
a8e39acb81 ASoC: qcom: Add MSM8998 sound card support
Add MSM8998 sound support: this driver supports basic functionality
and headphone jack.

Signed-off-by: AngeloGioacchino Del Regno <angelogioacchino.delregno@somainline.org>
(JAMI: fixup for 5.17)
2022-03-29 22:52:44 +03:00